diff options
Diffstat (limited to 'test/CodeGen/avx512f-builtins.c')
| -rw-r--r-- | test/CodeGen/avx512f-builtins.c | 427 |
1 files changed, 244 insertions, 183 deletions
diff --git a/test/CodeGen/avx512f-builtins.c b/test/CodeGen/avx512f-builtins.c index 5154e820bd..eedd3fc9e2 100644 --- a/test/CodeGen/avx512f-builtins.c +++ b/test/CodeGen/avx512f-builtins.c @@ -1,4 +1,5 @@ // RUN: %clang_cc1 -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512f -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -fms-extensions -fms-compatibility -ffreestanding %s -triple=x86_64-windows-msvc -target-feature +avx512f -emit-llvm -o - -Wall -Werror | FileCheck %s #include <immintrin.h> @@ -5019,137 +5020,197 @@ __m512 test_mm512_maskz_cvt_roundph_ps(__mmask16 __U, __m256i __A) return _mm512_maskz_cvt_roundph_ps(__U, __A, _MM_FROUND_CUR_DIRECTION); } +__m512 test_mm512_cvt_roundepi32_ps( __m512i __A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundepi32_ps + // CHECK: @llvm.x86.avx512.sitofp.round.v16f32.v16i32 + return _mm512_cvt_roundepi32_ps(__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + __m512 test_mm512_mask_cvt_roundepi32_ps(__m512 __W, __mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundepi32_ps - // CHECK: @llvm.x86.avx512.mask.cvtdq2ps.512 - return _mm512_mask_cvt_roundepi32_ps(__W,__U,__A,4); + // CHECK: @llvm.x86.avx512.sitofp.round.v16f32.v16i32 + // CHECK: select <16 x i1> %{{.*}}, <16 x float> %{{.*}}, <16 x float> %{{.*}} + return _mm512_mask_cvt_roundepi32_ps(__W,__U,__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512 test_mm512_maskz_cvt_roundepi32_ps(__mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundepi32_ps - // CHECK: @llvm.x86.avx512.mask.cvtdq2ps.512 - return _mm512_maskz_cvt_roundepi32_ps(__U,__A,4); + // CHECK: @llvm.x86.avx512.sitofp.round.v16f32.v16i32 + // CHECK: select <16 x i1> %{{.*}}, <16 x float> %{{.*}}, <16 x float> %{{.*}} + return _mm512_maskz_cvt_roundepi32_ps(__U,__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m512 test_mm512_cvt_roundepu32_ps(__m512i __A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundepu32_ps + // CHECK: @llvm.x86.avx512.uitofp.round.v16f32.v16i32 + return _mm512_cvt_roundepu32_ps(__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512 test_mm512_mask_cvt_roundepu32_ps(__m512 __W, __mmask16 __U,__m512i __A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundepu32_ps - // CHECK: @llvm.x86.avx512.mask.cvtudq2ps.512 - return _mm512_mask_cvt_roundepu32_ps(__W,__U,__A,4); + // CHECK: @llvm.x86.avx512.uitofp.round.v16f32.v16i32 + // CHECK: select <16 x i1> %{{.*}}, <16 x float> %{{.*}}, <16 x float> %{{.*}} + return _mm512_mask_cvt_roundepu32_ps(__W,__U,__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512 test_mm512_maskz_cvt_roundepu32_ps(__mmask16 __U,__m512i __A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundepu32_ps - // CHECK: @llvm.x86.avx512.mask.cvtudq2ps.512 - return _mm512_maskz_cvt_roundepu32_ps(__U,__A,4); + // CHECK: @llvm.x86.avx512.uitofp.round.v16f32.v16i32 + // CHECK: select <16 x i1> %{{.*}}, <16 x float> %{{.*}}, <16 x float> %{{.*}} + return _mm512_maskz_cvt_roundepu32_ps(__U,__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m256 test_mm512_cvt_roundpd_ps(__m512d A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundpd_ps + // CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512 + return _mm512_cvt_roundpd_ps(A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256 test_mm512_mask_cvt_roundpd_ps(__m256 W, __mmask8 U,__m512d A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundpd_ps // CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512 - return _mm512_mask_cvt_roundpd_ps(W,U,A,4); + return _mm512_mask_cvt_roundpd_ps(W,U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256 test_mm512_maskz_cvt_roundpd_ps(__mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_ps // CHECK: @llvm.x86.avx512.mask.cvtpd2ps.512 - return _mm512_maskz_cvt_roundpd_ps(U,A,4); + return _mm512_maskz_cvt_roundpd_ps(U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_cvtt_roundpd_epi32(__m512d A) { // CHECK-LABEL: @test_mm512_cvtt_roundpd_epi32 // CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512 - return _mm512_cvtt_roundpd_epi32(A,4); + return _mm512_cvtt_roundpd_epi32(A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_mask_cvtt_roundpd_epi32(__m256i W, __mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_mask_cvtt_roundpd_epi32 // CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512 - return _mm512_mask_cvtt_roundpd_epi32(W,U,A,4); + return _mm512_mask_cvtt_roundpd_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_maskz_cvtt_roundpd_epi32(__mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_maskz_cvtt_roundpd_epi32 // CHECK: @llvm.x86.avx512.mask.cvttpd2dq.512 - return _mm512_maskz_cvtt_roundpd_epi32(U,A,4); + return _mm512_maskz_cvtt_roundpd_epi32(U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m512i test_mm512_cvtt_roundps_epi32(__m512 A) +{ + // CHECK-LABEL: @test_mm512_cvtt_roundps_epi32 + // CHECK: @llvm.x86.avx512.mask.cvttps2dq.512 + return _mm512_cvtt_roundps_epi32(A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_mask_cvtt_roundps_epi32(__m512i W,__mmask16 U, __m512 A) { // CHECK-LABEL: @test_mm512_mask_cvtt_roundps_epi32 // CHECK: @llvm.x86.avx512.mask.cvttps2dq.512 - return _mm512_mask_cvtt_roundps_epi32(W,U,A,4); + return _mm512_mask_cvtt_roundps_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_maskz_cvtt_roundps_epi32(__mmask16 U, __m512 A) { // CHECK-LABEL: @test_mm512_maskz_cvtt_roundps_epi32 // CHECK: @llvm.x86.avx512.mask.cvttps2dq.512 - return _mm512_maskz_cvtt_roundps_epi32(U,A,4); + return _mm512_maskz_cvtt_roundps_epi32(U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m512i test_mm512_cvt_roundps_epi32(__m512 __A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundps_epi32 + // CHECK: @llvm.x86.avx512.mask.cvtps2dq.512 + return _mm512_cvt_roundps_epi32(__A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_mask_cvt_roundps_epi32(__m512i __W,__mmask16 __U,__m512 __A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundps_epi32 // CHECK: @llvm.x86.avx512.mask.cvtps2dq.512 - return _mm512_mask_cvt_roundps_epi32(__W,__U,__A,4); + return _mm512_mask_cvt_roundps_epi32(__W,__U,__A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_maskz_cvt_roundps_epi32(__mmask16 __U, __m512 __A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundps_epi32 // CHECK: @llvm.x86.avx512.mask.cvtps2dq.512 - return _mm512_maskz_cvt_roundps_epi32(__U,__A,4); + return _mm512_maskz_cvt_roundps_epi32(__U,__A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m256i test_mm512_cvt_roundpd_epi32(__m512d A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundpd_epi32 + // CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512 + return _mm512_cvt_roundpd_epi32(A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_mask_cvt_roundpd_epi32(__m256i W,__mmask8 U,__m512d A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundpd_epi32 // CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512 - return _mm512_mask_cvt_roundpd_epi32(W,U,A,4); + return _mm512_mask_cvt_roundpd_epi32(W,U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_maskz_cvt_roundpd_epi32(__mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_epi32 // CHECK: @llvm.x86.avx512.mask.cvtpd2dq.512 - return _mm512_maskz_cvt_roundpd_epi32(U,A,4); + return _mm512_maskz_cvt_roundpd_epi32(U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m512i test_mm512_cvt_roundps_epu32(__m512 __A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundps_epu32 + // CHECK: @llvm.x86.avx512.mask.cvtps2udq.512 + return _mm512_cvt_roundps_epu32(__A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_mask_cvt_roundps_epu32(__m512i __W,__mmask16 __U,__m512 __A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundps_epu32 // CHECK: @llvm.x86.avx512.mask.cvtps2udq.512 - return _mm512_mask_cvt_roundps_epu32(__W,__U,__A,4); + return _mm512_mask_cvt_roundps_epu32(__W,__U,__A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512i test_mm512_maskz_cvt_roundps_epu32(__mmask16 __U,__m512 __A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundps_epu32 // CHECK: @llvm.x86.avx512.mask.cvtps2udq.512 - return _mm512_maskz_cvt_roundps_epu32(__U,__A, 4); + return _mm512_maskz_cvt_roundps_epu32(__U,__A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); +} + +__m256i test_mm512_cvt_roundpd_epu32(__m512d A) +{ + // CHECK-LABEL: @test_mm512_cvt_roundpd_epu32 + // CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512 + return _mm512_cvt_roundpd_epu32(A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_mask_cvt_roundpd_epu32(__m256i W, __mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_mask_cvt_roundpd_epu32 // CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512 - return _mm512_mask_cvt_roundpd_epu32(W,U,A,4); + return _mm512_mask_cvt_roundpd_epu32(W,U,A,_MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m256i test_mm512_maskz_cvt_roundpd_epu32(__mmask8 U, __m512d A) { // CHECK-LABEL: @test_mm512_maskz_cvt_roundpd_epu32 // CHECK: @llvm.x86.avx512.mask.cvtpd2udq.512 - return _mm512_maskz_cvt_roundpd_epu32(U, A, 4); + return _mm512_maskz_cvt_roundpd_epu32(U, A, _MM_FROUND_TO_NEAREST_INT | _MM_FROUND_NO_EXC); } __m512 test_mm512_mask2_permutex2var_ps(__m512 __A, __m512i __I, __mmask16 __U, __m512 __B) { @@ -7002,193 +7063,193 @@ __m512 test_mm512_maskz_getexp_ps(__mmask16 __U, __m512 __A) { __m256 test_mm512_i64gather_ps(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i64gather_ps - // CHECK: @llvm.x86.avx512.gather.qps.512 + // CHECK: @llvm.x86.avx512.mask.gather.qps.512 return _mm512_i64gather_ps(__index, __addr, 2); } __m256 test_mm512_mask_i64gather_ps(__m256 __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i64gather_ps - // CHECK: @llvm.x86.avx512.gather.qps.512 + // CHECK: @llvm.x86.avx512.mask.gather.qps.512 return _mm512_mask_i64gather_ps(__v1_old, __mask, __index, __addr, 2); } __m256i test_mm512_i64gather_epi32(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i64gather_epi32 - // CHECK: @llvm.x86.avx512.gather.qpi.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpi.512 return _mm512_i64gather_epi32(__index, __addr, 2); } __m256i test_mm512_mask_i64gather_epi32(__m256i __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i64gather_epi32 - // CHECK: @llvm.x86.avx512.gather.qpi.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpi.512 return _mm512_mask_i64gather_epi32(__v1_old, __mask, __index, __addr, 2); } __m512d test_mm512_i64gather_pd(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i64gather_pd - // CHECK: @llvm.x86.avx512.gather.qpd.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpd.512 return _mm512_i64gather_pd(__index, __addr, 2); } __m512d test_mm512_mask_i64gather_pd(__m512d __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i64gather_pd - // CHECK: @llvm.x86.avx512.gather.qpd.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpd.512 return _mm512_mask_i64gather_pd(__v1_old, __mask, __index, __addr, 2); } __m512i test_mm512_i64gather_epi64(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i64gather_epi64 - // CHECK: @llvm.x86.avx512.gather.qpq.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpq.512 return _mm512_i64gather_epi64(__index, __addr, 2); } __m512i test_mm512_mask_i64gather_epi64(__m512i __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i64gather_epi64 - // CHECK: @llvm.x86.avx512.gather.qpq.512 + // CHECK: @llvm.x86.avx512.mask.gather.qpq.512 return _mm512_mask_i64gather_epi64(__v1_old, __mask, __index, __addr, 2); } __m512 test_mm512_i32gather_ps(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i32gather_ps - // CHECK: @llvm.x86.avx512.gather.dps.512 + // CHECK: @llvm.x86.avx512.mask.gather.dps.512 return _mm512_i32gather_ps(__index, __addr, 2); } __m512 test_mm512_mask_i32gather_ps(__m512 v1_old, __mmask16 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i32gather_ps - // CHECK: @llvm.x86.avx512.gather.dps.512 + // CHECK: @llvm.x86.avx512.mask.gather.dps.512 return _mm512_mask_i32gather_ps(v1_old, __mask, __index, __addr, 2); } __m512i test_mm512_i32gather_epi32(__m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i32gather_epi32 - // CHECK: @llvm.x86.avx512.gather.dpi.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpi.512 return _mm512_i32gather_epi32(__index, __addr, 2); } __m512i test_mm512_mask_i32gather_epi32(__m512i __v1_old, __mmask16 __mask, __m512i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i32gather_epi32 - // CHECK: @llvm.x86.avx512.gather.dpi.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpi.512 return _mm512_mask_i32gather_epi32(__v1_old, __mask, __index, __addr, 2); } __m512d test_mm512_i32gather_pd(__m256i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i32gather_pd - // CHECK: @llvm.x86.avx512.gather.dpd.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpd.512 return _mm512_i32gather_pd(__index, __addr, 2); } __m512d test_mm512_mask_i32gather_pd(__m512d __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i32gather_pd - // CHECK: @llvm.x86.avx512.gather.dpd.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpd.512 return _mm512_mask_i32gather_pd(__v1_old, __mask, __index, __addr, 2); } __m512i test_mm512_i32gather_epi64(__m256i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_i32gather_epi64 - // CHECK: @llvm.x86.avx512.gather.dpq.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpq.512 return _mm512_i32gather_epi64(__index, __addr, 2); } __m512i test_mm512_mask_i32gather_epi64(__m512i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) { // CHECK-LABEL: @test_mm512_mask_i32gather_epi64 - // CHECK: @llvm.x86.avx512.gather.dpq.512 + // CHECK: @llvm.x86.avx512.mask.gather.dpq.512 return _mm512_mask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2); } void test_mm512_i64scatter_ps(void *__addr, __m512i __index, __m256 __v1) { // CHECK-LABEL: @test_mm512_i64scatter_ps - // CHECK: @llvm.x86.avx512.scatter.qps.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qps.512 return _mm512_i64scatter_ps(__addr, __index, __v1, 2); } void test_mm512_mask_i64scatter_ps(void *__addr, __mmask8 __mask, __m512i __index, __m256 __v1) { // CHECK-LABEL: @test_mm512_mask_i64scatter_ps - // CHECK: @llvm.x86.avx512.scatter.qps.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qps.512 return _mm512_mask_i64scatter_ps(__addr, __mask, __index, __v1, 2); } void test_mm512_i64scatter_epi32(void *__addr, __m512i __index, __m256i __v1) { // CHECK-LABEL: @test_mm512_i64scatter_epi32 - // CHECK: @llvm.x86.avx512.scatter.qpi.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpi.512 return _mm512_i64scatter_epi32(__addr, __index, __v1, 2); } void test_mm512_mask_i64scatter_epi32(void *__addr, __mmask8 __mask, __m512i __index, __m256i __v1) { // CHECK-LABEL: @test_mm512_mask_i64scatter_epi32 - // CHECK: @llvm.x86.avx512.scatter.qpi.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpi.512 return _mm512_mask_i64scatter_epi32(__addr, __mask, __index, __v1, 2); } void test_mm512_i64scatter_pd(void *__addr, __m512i __index, __m512d __v1) { // CHECK-LABEL: @test_mm512_i64scatter_pd - // CHECK: @llvm.x86.avx512.scatter.qpd.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpd.512 return _mm512_i64scatter_pd(__addr, __index, __v1, 2); } void test_mm512_mask_i64scatter_pd(void *__addr, __mmask8 __mask, __m512i __index, __m512d __v1) { // CHECK-LABEL: @test_mm512_mask_i64scatter_pd - // CHECK: @llvm.x86.avx512.scatter.qpd.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpd.512 return _mm512_mask_i64scatter_pd(__addr, __mask, __index, __v1, 2); } void test_mm512_i64scatter_epi64(void *__addr, __m512i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_i64scatter_epi64 - // CHECK: @llvm.x86.avx512.scatter.qpq.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpq.512 return _mm512_i64scatter_epi64(__addr, __index, __v1, 2); } void test_mm512_mask_i64scatter_epi64(void *__addr, __mmask8 __mask, __m512i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_mask_i64scatter_epi64 - // CHECK: @llvm.x86.avx512.scatter.qpq.512 + // CHECK: @llvm.x86.avx512.mask.scatter.qpq.512 return _mm512_mask_i64scatter_epi64(__addr, __mask, __index, __v1, 2); } void test_mm512_i32scatter_ps(void *__addr, __m512i __index, __m512 __v1) { // CHECK-LABEL: @test_mm512_i32scatter_ps - // CHECK: @llvm.x86.avx512.scatter.dps.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dps.512 return _mm512_i32scatter_ps(__addr, __index, __v1, 2); } void test_mm512_mask_i32scatter_ps(void *__addr, __mmask16 __mask, __m512i __index, __m512 __v1) { // CHECK-LABEL: @test_mm512_mask_i32scatter_ps - // CHECK: @llvm.x86.avx512.scatter.dps.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dps.512 return _mm512_mask_i32scatter_ps(__addr, __mask, __index, __v1, 2); } void test_mm512_i32scatter_epi32(void *__addr, __m512i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_i32scatter_epi32 - // CHECK: @llvm.x86.avx512.scatter.dpi.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpi.512 return _mm512_i32scatter_epi32(__addr, __index, __v1, 2); } void test_mm512_mask_i32scatter_epi32(void *__addr, __mmask16 __mask, __m512i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_mask_i32scatter_epi32 - // CHECK: @llvm.x86.avx512.scatter.dpi.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpi.512 return _mm512_mask_i32scatter_epi32(__addr, __mask, __index, __v1, 2); } void test_mm512_i32scatter_pd(void *__addr, __m256i __index, __m512d __v1) { // CHECK-LABEL: @test_mm512_i32scatter_pd - // CHECK: @llvm.x86.avx512.scatter.dpd.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpd.512 return _mm512_i32scatter_pd(__addr, __index, __v1, 2); } void test_mm512_mask_i32scatter_pd(void *__addr, __mmask8 __mask, __m256i __index, __m512d __v1) { // CHECK-LABEL: @test_mm512_mask_i32scatter_pd - // CHECK: @llvm.x86.avx512.scatter.dpd.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpd.512 return _mm512_mask_i32scatter_pd(__addr, __mask, __index, __v1, 2); } void test_mm512_i32scatter_epi64(void *__addr, __m256i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_i32scatter_epi64 - // CHECK: @llvm.x86.avx512.scatter.dpq.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpq.512 return _mm512_i32scatter_epi64(__addr, __index, __v1, 2); } void test_mm512_mask_i32scatter_epi64(void *__addr, __mmask8 __mask, __m256i __index, __m512i __v1) { // CHECK-LABEL: @test_mm512_mask_i32scatter_epi64 - // CHECK: @llvm.x86.avx512.scatter.dpq.512 + // CHECK: @llvm.x86.avx512.mask.scatter.dpq.512 return _mm512_mask_i32scatter_epi64(__addr, __mask, __index, __v1, 2); } @@ -8534,49 +8595,49 @@ void test_mm512_stream_ps(float *__P, __m512 __A) { __m512d test_mm512_mask_compress_pd(__m512d __W, __mmask8 __U, __m512d __A) { // CHECK-LABEL: @test_mm512_mask_compress_pd - // CHECK: @llvm.x86.avx512.mask.compress.pd.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_mask_compress_pd(__W, __U, __A); } __m512d test_mm512_maskz_compress_pd(__mmask8 __U, __m512d __A) { // CHECK-LABEL: @test_mm512_maskz_compress_pd - // CHECK: @llvm.x86.avx512.mask.compress.pd.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_maskz_compress_pd(__U, __A); } __m512i test_mm512_mask_compress_epi64(__m512i __W, __mmask8 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_mask_compress_epi64 - // CHECK: @llvm.x86.avx512.mask.compress.q.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_mask_compress_epi64(__W, __U, __A); } __m512i test_mm512_maskz_compress_epi64(__mmask8 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_maskz_compress_epi64 - // CHECK: @llvm.x86.avx512.mask.compress.q.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_maskz_compress_epi64(__U, __A); } __m512 test_mm512_mask_compress_ps(__m512 __W, __mmask16 __U, __m512 __A) { // CHECK-LABEL: @test_mm512_mask_compress_ps - // CHECK: @llvm.x86.avx512.mask.compress.ps.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_mask_compress_ps(__W, __U, __A); } __m512 test_mm512_maskz_compress_ps(__mmask16 __U, __m512 __A) { // CHECK-LABEL: @test_mm512_maskz_compress_ps - // CHECK: @llvm.x86.avx512.mask.compress.ps.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_maskz_compress_ps(__U, __A); } __m512i test_mm512_mask_compress_epi32(__m512i __W, __mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_mask_compress_epi32 - // CHECK: @llvm.x86.avx512.mask.compress.d.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_mask_compress_epi32(__W, __U, __A); } __m512i test_mm512_maskz_compress_epi32(__mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_maskz_compress_epi32 - // CHECK: @llvm.x86.avx512.mask.compress.d.512 + // CHECK: @llvm.x86.avx512.mask.compress return _mm512_maskz_compress_epi32(__U, __A); } @@ -8690,25 +8751,25 @@ __m512i test_mm512_maskz_shuffle_epi32(__mmask16 __U, __m512i __A) { __m512d test_mm512_mask_expand_pd(__m512d __W, __mmask8 __U, __m512d __A) { // CHECK-LABEL: @test_mm512_mask_expand_pd - // CHECK: @llvm.x86.avx512.mask.expand.pd.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_mask_expand_pd(__W, __U, __A); } __m512d test_mm512_maskz_expand_pd(__mmask8 __U, __m512d __A) { // CHECK-LABEL: @test_mm512_maskz_expand_pd - // CHECK: @llvm.x86.avx512.mask.expand.pd.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_maskz_expand_pd(__U, __A); } __m512i test_mm512_mask_expand_epi64(__m512i __W, __mmask8 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_mask_expand_epi64 - // CHECK: @llvm.x86.avx512.mask.expand.q.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_mask_expand_epi64(__W, __U, __A); } __m512i test_mm512_maskz_expand_epi64(__mmask8 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_maskz_expand_epi64 - // CHECK: @llvm.x86.avx512.mask.expand.q.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_maskz_expand_epi64(__U, __A); } __m512i test_mm512_mask_expandloadu_epi64(__m512i __W, __mmask8 __U, void const *__P) { @@ -8761,25 +8822,25 @@ __m512 test_mm512_maskz_expandloadu_ps(__mmask16 __U, void const *__P) { __m512 test_mm512_mask_expand_ps(__m512 __W, __mmask16 __U, __m512 __A) { // CHECK-LABEL: @test_mm512_mask_expand_ps - // CHECK: @llvm.x86.avx512.mask.expand.ps.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_mask_expand_ps(__W, __U, __A); } __m512 test_mm512_maskz_expand_ps(__mmask16 __U, __m512 __A) { // CHECK-LABEL: @test_mm512_maskz_expand_ps - // CHECK: @llvm.x86.avx512.mask.expand.ps.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_maskz_expand_ps(__U, __A); } __m512i test_mm512_mask_expand_epi32(__m512i __W, __mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_mask_expand_epi32 - // CHECK: @llvm.x86.avx512.mask.expand.d.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_mask_expand_epi32(__W, __U, __A); } __m512i test_mm512_maskz_expand_epi32(__mmask16 __U, __m512i __A) { // CHECK-LABEL: @test_mm512_maskz_expand_epi32 - // CHECK: @llvm.x86.avx512.mask.expand.d.512 + // CHECK: @llvm.x86.avx512.mask.expand return _mm512_maskz_expand_epi32(__U, __A); } __m512d test_mm512_cvt_roundps_pd(__m256 __A) { @@ -10079,70 +10140,70 @@ __m512i test_mm512_set_epi8(char e63, char e62, char e61, char e60, char e59, char e1, char e0) { //CHECK-LABEL: @test_mm512_set_epi8 - //CHECK: load i8, i8* %e63.addr, align 1 - //CHECK: load i8, i8* %e62.addr, align 1 - //CHECK: load i8, i8* %e61.addr, align 1 - //CHECK: load i8, i8* %e60.addr, align 1 - //CHECK: load i8, i8* %e59.addr, align 1 - //CHECK: load i8, i8* %e58.addr, align 1 - //CHECK: load i8, i8* %e57.addr, align 1 - //CHECK: load i8, i8* %e56.addr, align 1 - //CHECK: load i8, i8* %e55.addr, align 1 - //CHECK: load i8, i8* %e54.addr, align 1 - //CHECK: load i8, i8* %e53.addr, align 1 - //CHECK: load i8, i8* %e52.addr, align 1 - //CHECK: load i8, i8* %e51.addr, align 1 - //CHECK: load i8, i8* %e50.addr, align 1 - //CHECK: load i8, i8* %e49.addr, align 1 - //CHECK: load i8, i8* %e48.addr, align 1 - //CHECK: load i8, i8* %e47.addr, align 1 - //CHECK: load i8, i8* %e46.addr, align 1 - //CHECK: load i8, i8* %e45.addr, align 1 - //CHECK: load i8, i8* %e44.addr, align 1 - //CHECK: load i8, i8* %e43.addr, align 1 - //CHECK: load i8, i8* %e42.addr, align 1 - //CHECK: load i8, i8* %e41.addr, align 1 - //CHECK: load i8, i8* %e40.addr, align 1 - //CHECK: load i8, i8* %e39.addr, align 1 - //CHECK: load i8, i8* %e38.addr, align 1 - //CHECK: load i8, i8* %e37.addr, align 1 - //CHECK: load i8, i8* %e36.addr, align 1 - //CHECK: load i8, i8* %e35.addr, align 1 - //CHECK: load i8, i8* %e34.addr, align 1 - //CHECK: load i8, i8* %e33.addr, align 1 - //CHECK: load i8, i8* %e32.addr, align 1 - //CHECK: load i8, i8* %e31.addr, align 1 - //CHECK: load i8, i8* %e30.addr, align 1 - //CHECK: load i8, i8* %e29.addr, align 1 - //CHECK: load i8, i8* %e28.addr, align 1 - //CHECK: load i8, i8* %e27.addr, align 1 - //CHECK: load i8, i8* %e26.addr, align 1 - //CHECK: load i8, i8* %e25.addr, align 1 - //CHECK: load i8, i8* %e24.addr, align 1 - //CHECK: load i8, i8* %e23.addr, align 1 - //CHECK: load i8, i8* %e22.addr, align 1 - //CHECK: load i8, i8* %e21.addr, align 1 - //CHECK: load i8, i8* %e20.addr, align 1 - //CHECK: load i8, i8* %e19.addr, align 1 - //CHECK: load i8, i8* %e18.addr, align 1 - //CHECK: load i8, i8* %e17.addr, align 1 - //CHECK: load i8, i8* %e16.addr, align 1 - //CHECK: load i8, i8* %e15.addr, align 1 - //CHECK: load i8, i8* %e14.addr, align 1 - //CHECK: load i8, i8* %e13.addr, align 1 - //CHECK: load i8, i8* %e12.addr, align 1 - //CHECK: load i8, i8* %e11.addr, align 1 - //CHECK: load i8, i8* %e10.addr, align 1 - //CHECK: load i8, i8* %e9.addr, align 1 - //CHECK: load i8, i8* %e8.addr, align 1 - //CHECK: load i8, i8* %e7.addr, align 1 - //CHECK: load i8, i8* %e6.addr, align 1 - //CHECK: load i8, i8* %e5.addr, align 1 - //CHECK: load i8, i8* %e4.addr, align 1 - //CHECK: load i8, i8* %e3.addr, align 1 - //CHECK: load i8, i8* %e2.addr, align 1 - //CHECK: load i8, i8* %e1.addr, align 1 - //CHECK: load i8, i8* %e0.addr, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 + //CHECK: load i8, i8* %{{.*}}, align 1 return _mm512_set_epi8(e63, e62, e61, e60, e59, e58, e57, e56, e55, e54, e53, e52, e51, e50, e49, e48,e47, e46, e45, e44, e43, e42, e41, e40, e39, e38, e37, e36, e35, e34, e33, e32,e31, e30, e29, e28, e27, e26, @@ -10226,22 +10287,22 @@ __m512i test_mm512_setr_epi32 (int __A, int __B, int __C, int __D, int __M, int __N, int __O, int __P) { //CHECK-LABEL: @test_mm512_setr_epi32 - //CHECK: load{{.*}}%__P.addr, align 4 - //CHECK: load{{.*}}%__O.addr, align 4 - //CHECK: load{{.*}}%__N.addr, align 4 - //CHECK: load{{.*}}%__M.addr, align 4 - //CHECK: load{{.*}}%__L.addr, align 4 - //CHECK: load{{.*}}%__K.addr, align 4 - //CHECK: load{{.*}}%__J.addr, align 4 - //CHECK: load{{.*}}%__I.addr, align 4 - //CHECK: load{{.*}}%__H.addr, align 4 - //CHECK: load{{.*}}%__G.addr, align 4 - //CHECK: load{{.*}}%__F.addr, align 4 - //CHECK: load{{.*}}%__E.addr, align 4 - //CHECK: load{{.*}}%__D.addr, align 4 - //CHECK: load{{.*}}%__C.addr, align 4 - //CHECK: load{{.*}}%__B.addr, align 4 - //CHECK: load{{.*}}%__A.addr, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 //CHECK: insertelement{{.*}}i32 0 //CHECK: insertelement{{.*}}i32 1 //CHECK: insertelement{{.*}}i32 2 @@ -10314,14 +10375,14 @@ __m512i test_mm512_setr_epi64 (long long __A, long long __B, long long __C, long long __G, long long __H) { //CHECK-LABEL: @test_mm512_setr_epi64 - //CHECK: load{{.*}}%__H.addr, align 8 - //CHECK: load{{.*}}%__G.addr, align 8 - //CHECK: load{{.*}}%__F.addr, align 8 - //CHECK: load{{.*}}%__E.addr, align 8 - //CHECK: load{{.*}}%__D.addr, align 8 - //CHECK: load{{.*}}%__C.addr, align 8 - //CHECK: load{{.*}}%__B.addr, align 8 - //CHECK: load{{.*}}%__A.addr, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 //CHECK: insertelement{{.*}}i32 0 //CHECK: insertelement{{.*}}i32 1 //CHECK: insertelement{{.*}}i32 2 @@ -10352,14 +10413,14 @@ __m512d test_mm512_setr_pd (double __A, double __B, double __C, double __D, double __E, double __F, double __G, double __H) { //CHECK-LABEL: @test_mm512_setr_pd - //CHECK: load{{.*}}%__H.addr, align 8 - //CHECK: load{{.*}}%__G.addr, align 8 - //CHECK: load{{.*}}%__F.addr, align 8 - //CHECK: load{{.*}}%__E.addr, align 8 - //CHECK: load{{.*}}%__D.addr, align 8 - //CHECK: load{{.*}}%__C.addr, align 8 - //CHECK: load{{.*}}%__B.addr, align 8 - //CHECK: load{{.*}}%__A.addr, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 + //CHECK: load{{.*}}%{{.*}}, align 8 //CHECK: insertelement{{.*}}i32 0 //CHECK: insertelement{{.*}}i32 1 //CHECK: insertelement{{.*}}i32 2 @@ -10443,22 +10504,22 @@ __m512 test_mm512_setr_ps (float __A, float __B, float __C, float __D, float __M, float __N, float __O, float __P) { //CHECK-LABEL: @test_mm512_setr_ps - //CHECK: load{{.*}}%__P.addr, align 4 - //CHECK: load{{.*}}%__O.addr, align 4 - //CHECK: load{{.*}}%__N.addr, align 4 - //CHECK: load{{.*}}%__M.addr, align 4 - //CHECK: load{{.*}}%__L.addr, align 4 - //CHECK: load{{.*}}%__K.addr, align 4 - //CHECK: load{{.*}}%__J.addr, align 4 - //CHECK: load{{.*}}%__I.addr, align 4 - //CHECK: load{{.*}}%__H.addr, align 4 - //CHECK: load{{.*}}%__G.addr, align 4 - //CHECK: load{{.*}}%__F.addr, align 4 - //CHECK: load{{.*}}%__E.addr, align 4 - //CHECK: load{{.*}}%__D.addr, align 4 - //CHECK: load{{.*}}%__C.addr, align 4 - //CHECK: load{{.*}}%__B.addr, align 4 - //CHECK: load{{.*}}%__A.addr, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 + //CHECK: load{{.*}}%{{.*}}, align 4 //CHECK: insertelement{{.*}}i32 0 //CHECK: insertelement{{.*}}i32 1 //CHECK: insertelement{{.*}}i32 2 |