Author: Simon Pilgrim Date: 2025-08-15T09:44:18+01:00 New Revision: b014d10ed7a1ec9864016a9db0e7323857bc2a3f
URL: https://github.com/llvm/llvm-project/commit/b014d10ed7a1ec9864016a9db0e7323857bc2a3f DIFF: https://github.com/llvm/llvm-project/commit/b014d10ed7a1ec9864016a9db0e7323857bc2a3f.diff LOG: [X86] avx512cd-builtins.c + avx512vlcd-builtins.c - add C/C++ and 32/64-bit test coverage Added: Modified: clang/test/CodeGen/X86/avx512cd-builtins.c clang/test/CodeGen/X86/avx512vlcd-builtins.c Removed: ################################################################################ diff --git a/clang/test/CodeGen/X86/avx512cd-builtins.c b/clang/test/CodeGen/X86/avx512cd-builtins.c index 3c1415cd62565..45df0fccb322f 100644 --- a/clang/test/CodeGen/X86/avx512cd-builtins.c +++ b/clang/test/CodeGen/X86/avx512cd-builtins.c @@ -1,79 +1,82 @@ -// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s #include <immintrin.h> __m512i test_mm512_conflict_epi64(__m512i __A) { - // CHECK-LABEL: @test_mm512_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.512 + // CHECK-LABEL: test_mm512_conflict_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.x86.avx512.conflict.q.512(<8 x i64> %{{.*}}) return _mm512_conflict_epi64(__A); } __m512i test_mm512_mask_conflict_epi64(__m512i __W, __mmask8 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_mask_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.512 + // CHECK-LABEL: test_mm512_mask_conflict_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.x86.avx512.conflict.q.512(<8 x i64> %{{.*}}) // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} return _mm512_mask_conflict_epi64(__W,__U,__A); } __m512i test_mm512_maskz_conflict_epi64(__mmask8 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_maskz_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.512 + // CHECK-LABEL: test_mm512_maskz_conflict_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.x86.avx512.conflict.q.512(<8 x i64> %{{.*}}) // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} return _mm512_maskz_conflict_epi64(__U,__A); } __m512i test_mm512_conflict_epi32(__m512i __A) { - // CHECK-LABEL: @test_mm512_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.512 + // CHECK-LABEL: test_mm512_conflict_epi32 + // CHECK: call <16 x i32> @llvm.x86.avx512.conflict.d.512(<16 x i32> %{{.*}}) return _mm512_conflict_epi32(__A); } __m512i test_mm512_mask_conflict_epi32(__m512i __W, __mmask16 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_mask_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.512 + // CHECK-LABEL: test_mm512_mask_conflict_epi32 + // CHECK: call <16 x i32> @llvm.x86.avx512.conflict.d.512(<16 x i32> %{{.*}}) // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} return _mm512_mask_conflict_epi32(__W,__U,__A); } __m512i test_mm512_maskz_conflict_epi32(__mmask16 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_maskz_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.512 + // CHECK-LABEL: test_mm512_maskz_conflict_epi32 + // CHECK: call <16 x i32> @llvm.x86.avx512.conflict.d.512(<16 x i32> %{{.*}}) // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} return _mm512_maskz_conflict_epi32(__U,__A); } __m512i test_mm512_lzcnt_epi32(__m512i __A) { - // CHECK-LABEL: @test_mm512_lzcnt_epi32 + // CHECK-LABEL: test_mm512_lzcnt_epi32 // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false) return _mm512_lzcnt_epi32(__A); } __m512i test_mm512_mask_lzcnt_epi32(__m512i __W, __mmask16 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_mask_lzcnt_epi32 + // CHECK-LABEL: test_mm512_mask_lzcnt_epi32 // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false) // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} return _mm512_mask_lzcnt_epi32(__W,__U,__A); } __m512i test_mm512_maskz_lzcnt_epi32(__mmask16 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_maskz_lzcnt_epi32 + // CHECK-LABEL: test_mm512_maskz_lzcnt_epi32 // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false) // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} return _mm512_maskz_lzcnt_epi32(__U,__A); } __m512i test_mm512_lzcnt_epi64(__m512i __A) { - // CHECK-LABEL: @test_mm512_lzcnt_epi64 - // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm512_lzcnt_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) return _mm512_lzcnt_epi64(__A); } __m512i test_mm512_mask_lzcnt_epi64(__m512i __W, __mmask8 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_mask_lzcnt_epi64 - // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm512_mask_lzcnt_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} return _mm512_mask_lzcnt_epi64(__W,__U,__A); } __m512i test_mm512_maskz_lzcnt_epi64(__mmask8 __U, __m512i __A) { - // CHECK-LABEL: @test_mm512_maskz_lzcnt_epi64 - // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm512_maskz_lzcnt_epi64 + // CHECK: call {{.*}}<8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false) // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}} return _mm512_maskz_lzcnt_epi64(__U,__A); } __m512i test_mm512_broadcastmb_epi64(__m512i a, __m512i b) { - // CHECK-LABEL: @test_mm512_broadcastmb_epi64 + // CHECK-LABEL: test_mm512_broadcastmb_epi64 // CHECK: icmp eq <8 x i64> %{{.*}}, %{{.*}} // CHECK: zext i8 %{{.*}} to i64 // CHECK: insertelement <8 x i64> poison, i64 %{{.*}}, i32 0 @@ -88,7 +91,7 @@ __m512i test_mm512_broadcastmb_epi64(__m512i a, __m512i b) { } __m512i test_mm512_broadcastmw_epi32(__m512i a, __m512i b) { - // CHECK-LABEL: @test_mm512_broadcastmw_epi32 + // CHECK-LABEL: test_mm512_broadcastmw_epi32 // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}} // CHECK: zext i16 %{{.*}} to i32 // CHECK: insertelement <16 x i32> poison, i32 %{{.*}} diff --git a/clang/test/CodeGen/X86/avx512vlcd-builtins.c b/clang/test/CodeGen/X86/avx512vlcd-builtins.c index b784809810e3d..939fd6460e6a6 100644 --- a/clang/test/CodeGen/X86/avx512vlcd-builtins.c +++ b/clang/test/CodeGen/X86/avx512vlcd-builtins.c @@ -1,10 +1,13 @@ -// RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s +// RUN: %clang_cc1 -x c++ -flax-vector-conversions=none -ffreestanding %s -triple=i386-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s #include <immintrin.h> __m128i test_mm_broadcastmb_epi64(__m128i a,__m128i b) { - // CHECK-LABEL: @test_mm_broadcastmb_epi64 + // CHECK-LABEL: test_mm_broadcastmb_epi64 // CHECK: icmp eq <4 x i32> %{{.*}}, %{{.*}} // CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7> // CHECK: zext i8 %{{.*}} to i64 @@ -14,7 +17,7 @@ __m128i test_mm_broadcastmb_epi64(__m128i a,__m128i b) { } __m256i test_mm256_broadcastmb_epi64(__m256i a, __m256i b) { - // CHECK-LABEL: @test_mm256_broadcastmb_epi64 + // CHECK-LABEL: test_mm256_broadcastmb_epi64 // CHECK: icmp eq <4 x i64> %{{.*}}, %{{.*}} // CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7> // CHECK: zext i8 %{{.*}} to i64 @@ -26,7 +29,7 @@ __m256i test_mm256_broadcastmb_epi64(__m256i a, __m256i b) { } __m128i test_mm_broadcastmw_epi32(__m512i a, __m512i b) { - // CHECK-LABEL: @test_mm_broadcastmw_epi32 + // CHECK-LABEL: test_mm_broadcastmw_epi32 // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}} // CHECK: zext i16 %{{.*}} to i32 // CHECK: insertelement <4 x i32> poison, i32 %{{.*}}, i32 0 @@ -37,7 +40,7 @@ __m128i test_mm_broadcastmw_epi32(__m512i a, __m512i b) { } __m256i test_mm256_broadcastmw_epi32(__m512i a, __m512i b) { - // CHECK-LABEL: @test_mm256_broadcastmw_epi32 + // CHECK-LABEL: test_mm256_broadcastmw_epi32 // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}} // CHECK: zext i16 %{{.*}} to i32 // CHECK: insertelement <8 x i32> poison, i32 %{{.*}}, i32 0 @@ -52,161 +55,161 @@ __m256i test_mm256_broadcastmw_epi32(__m512i a, __m512i b) { } __m128i test_mm_conflict_epi64(__m128i __A) { - // CHECK-LABEL: @test_mm_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.128 + // CHECK-LABEL: test_mm_conflict_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.x86.avx512.conflict.q.128(<2 x i64> %{{.*}}) return _mm_conflict_epi64(__A); } __m128i test_mm_mask_conflict_epi64(__m128i __W, __mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_mask_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.128 + // CHECK-LABEL: test_mm_mask_conflict_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.x86.avx512.conflict.q.128(<2 x i64> %{{.*}}) // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} return _mm_mask_conflict_epi64(__W, __U, __A); } __m128i test_mm_maskz_conflict_epi64(__mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_maskz_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.128 + // CHECK-LABEL: test_mm_maskz_conflict_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.x86.avx512.conflict.q.128(<2 x i64> %{{.*}}) // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} return _mm_maskz_conflict_epi64(__U, __A); } __m256i test_mm256_conflict_epi64(__m256i __A) { - // CHECK-LABEL: @test_mm256_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.256 + // CHECK-LABEL: test_mm256_conflict_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.x86.avx512.conflict.q.256(<4 x i64> %{{.*}}) return _mm256_conflict_epi64(__A); } __m256i test_mm256_mask_conflict_epi64(__m256i __W, __mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_mask_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.256 + // CHECK-LABEL: test_mm256_mask_conflict_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.x86.avx512.conflict.q.256(<4 x i64> %{{.*}}) // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} return _mm256_mask_conflict_epi64(__W, __U, __A); } __m256i test_mm256_maskz_conflict_epi64(__mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_maskz_conflict_epi64 - // CHECK: @llvm.x86.avx512.conflict.q.256 + // CHECK-LABEL: test_mm256_maskz_conflict_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.x86.avx512.conflict.q.256(<4 x i64> %{{.*}}) // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} return _mm256_maskz_conflict_epi64(__U, __A); } __m128i test_mm_conflict_epi32(__m128i __A) { - // CHECK-LABEL: @test_mm_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.128 + // CHECK-LABEL: test_mm_conflict_epi32 + // CHECK: call <4 x i32> @llvm.x86.avx512.conflict.d.128(<4 x i32> %{{.*}}) return _mm_conflict_epi32(__A); } __m128i test_mm_mask_conflict_epi32(__m128i __W, __mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_mask_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.128 + // CHECK-LABEL: test_mm_mask_conflict_epi32 + // CHECK: call <4 x i32> @llvm.x86.avx512.conflict.d.128(<4 x i32> %{{.*}}) // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} return _mm_mask_conflict_epi32(__W, __U, __A); } __m128i test_mm_maskz_conflict_epi32(__mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_maskz_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.128 + // CHECK-LABEL: test_mm_maskz_conflict_epi32 + // CHECK: call <4 x i32> @llvm.x86.avx512.conflict.d.128(<4 x i32> %{{.*}}) // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} return _mm_maskz_conflict_epi32(__U, __A); } __m256i test_mm256_conflict_epi32(__m256i __A) { - // CHECK-LABEL: @test_mm256_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.256 + // CHECK-LABEL: test_mm256_conflict_epi32 + // CHECK: call <8 x i32> @llvm.x86.avx512.conflict.d.256(<8 x i32> %{{.*}}) return _mm256_conflict_epi32(__A); } __m256i test_mm256_mask_conflict_epi32(__m256i __W, __mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_mask_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.256 + // CHECK-LABEL: test_mm256_mask_conflict_epi32 + // CHECK: call <8 x i32> @llvm.x86.avx512.conflict.d.256(<8 x i32> %{{.*}}) // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} return _mm256_mask_conflict_epi32(__W, __U, __A); } __m256i test_mm256_maskz_conflict_epi32(__mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_maskz_conflict_epi32 - // CHECK: @llvm.x86.avx512.conflict.d.256 + // CHECK-LABEL: test_mm256_maskz_conflict_epi32 + // CHECK: call <8 x i32> @llvm.x86.avx512.conflict.d.256(<8 x i32> %{{.*}}) // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} return _mm256_maskz_conflict_epi32(__U, __A); } __m128i test_mm_lzcnt_epi32(__m128i __A) { - // CHECK-LABEL: @test_mm_lzcnt_epi32 + // CHECK-LABEL: test_mm_lzcnt_epi32 // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false) return _mm_lzcnt_epi32(__A); } __m128i test_mm_mask_lzcnt_epi32(__m128i __W, __mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_mask_lzcnt_epi32 + // CHECK-LABEL: test_mm_mask_lzcnt_epi32 // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false) // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} return _mm_mask_lzcnt_epi32(__W, __U, __A); } __m128i test_mm_maskz_lzcnt_epi32(__mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_maskz_lzcnt_epi32 + // CHECK-LABEL: test_mm_maskz_lzcnt_epi32 // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false) // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}} return _mm_maskz_lzcnt_epi32(__U, __A); } __m256i test_mm256_lzcnt_epi32(__m256i __A) { - // CHECK-LABEL: @test_mm256_lzcnt_epi32 + // CHECK-LABEL: test_mm256_lzcnt_epi32 // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false) return _mm256_lzcnt_epi32(__A); } __m256i test_mm256_mask_lzcnt_epi32(__m256i __W, __mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_mask_lzcnt_epi32 + // CHECK-LABEL: test_mm256_mask_lzcnt_epi32 // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false) // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} return _mm256_mask_lzcnt_epi32(__W, __U, __A); } __m256i test_mm256_maskz_lzcnt_epi32(__mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_maskz_lzcnt_epi32 + // CHECK-LABEL: test_mm256_maskz_lzcnt_epi32 // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false) // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}} return _mm256_maskz_lzcnt_epi32(__U, __A); } __m128i test_mm_lzcnt_epi64(__m128i __A) { - // CHECK-LABEL: @test_mm_lzcnt_epi64 - // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm_lzcnt_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) return _mm_lzcnt_epi64(__A); } __m128i test_mm_mask_lzcnt_epi64(__m128i __W, __mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_mask_lzcnt_epi64 - // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm_mask_lzcnt_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} return _mm_mask_lzcnt_epi64(__W, __U, __A); } __m128i test_mm_maskz_lzcnt_epi64(__mmask8 __U, __m128i __A) { - // CHECK-LABEL: @test_mm_maskz_lzcnt_epi64 - // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm_maskz_lzcnt_epi64 + // CHECK: call {{.*}}<2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false) // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}} return _mm_maskz_lzcnt_epi64(__U, __A); } __m256i test_mm256_lzcnt_epi64(__m256i __A) { - // CHECK-LABEL: @test_mm256_lzcnt_epi64 - // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm256_lzcnt_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) return _mm256_lzcnt_epi64(__A); } __m256i test_mm256_mask_lzcnt_epi64(__m256i __W, __mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_mask_lzcnt_epi64 - // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm256_mask_lzcnt_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} return _mm256_mask_lzcnt_epi64(__W, __U, __A); } __m256i test_mm256_maskz_lzcnt_epi64(__mmask8 __U, __m256i __A) { - // CHECK-LABEL: @test_mm256_maskz_lzcnt_epi64 - // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) + // CHECK-LABEL: test_mm256_maskz_lzcnt_epi64 + // CHECK: call {{.*}}<4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false) // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}} return _mm256_maskz_lzcnt_epi64(__U, __A); } _______________________________________________ cfe-commits mailing list cfe-commits@lists.llvm.org https://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits
