1 // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vbmi -emit-llvm -o - -Wall -Werror | FileCheck %s
2
3
4 #include <immintrin.h>
5
test_mm512_mask2_permutex2var_epi8(__m512i __A,__m512i __I,__mmask64 __U,__m512i __B)6 __m512i test_mm512_mask2_permutex2var_epi8(__m512i __A, __m512i __I, __mmask64 __U, __m512i __B) {
7 // CHECK-LABEL: @test_mm512_mask2_permutex2var_epi8
8 // CHECK: @llvm.x86.avx512.vpermi2var.qi.512
9 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
10 return _mm512_mask2_permutex2var_epi8(__A, __I, __U, __B);
11 }
12
test_mm512_permutex2var_epi8(__m512i __A,__m512i __I,__m512i __B)13 __m512i test_mm512_permutex2var_epi8(__m512i __A, __m512i __I, __m512i __B) {
14 // CHECK-LABEL: @test_mm512_permutex2var_epi8
15 // CHECK: @llvm.x86.avx512.vpermi2var.qi.512
16 return _mm512_permutex2var_epi8(__A, __I, __B);
17 }
18
test_mm512_mask_permutex2var_epi8(__m512i __A,__mmask64 __U,__m512i __I,__m512i __B)19 __m512i test_mm512_mask_permutex2var_epi8(__m512i __A, __mmask64 __U, __m512i __I, __m512i __B) {
20 // CHECK-LABEL: @test_mm512_mask_permutex2var_epi8
21 // CHECK: @llvm.x86.avx512.vpermi2var.qi.512
22 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
23 return _mm512_mask_permutex2var_epi8(__A, __U, __I, __B);
24 }
25
test_mm512_maskz_permutex2var_epi8(__mmask64 __U,__m512i __A,__m512i __I,__m512i __B)26 __m512i test_mm512_maskz_permutex2var_epi8(__mmask64 __U, __m512i __A, __m512i __I, __m512i __B) {
27 // CHECK-LABEL: @test_mm512_maskz_permutex2var_epi8
28 // CHECK: @llvm.x86.avx512.vpermi2var.qi.512
29 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
30 return _mm512_maskz_permutex2var_epi8(__U, __A, __I, __B);
31 }
32
test_mm512_permutexvar_epi8(__m512i __A,__m512i __B)33 __m512i test_mm512_permutexvar_epi8(__m512i __A, __m512i __B) {
34 // CHECK-LABEL: @test_mm512_permutexvar_epi8
35 // CHECK: @llvm.x86.avx512.permvar.qi.512
36 return _mm512_permutexvar_epi8(__A, __B);
37 }
38
test_mm512_maskz_permutexvar_epi8(__mmask64 __M,__m512i __A,__m512i __B)39 __m512i test_mm512_maskz_permutexvar_epi8(__mmask64 __M, __m512i __A, __m512i __B) {
40 // CHECK-LABEL: @test_mm512_maskz_permutexvar_epi8
41 // CHECK: @llvm.x86.avx512.permvar.qi.512
42 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
43 return _mm512_maskz_permutexvar_epi8(__M, __A, __B);
44 }
45
test_mm512_mask_permutexvar_epi8(__m512i __W,__mmask64 __M,__m512i __A,__m512i __B)46 __m512i test_mm512_mask_permutexvar_epi8(__m512i __W, __mmask64 __M, __m512i __A, __m512i __B) {
47 // CHECK-LABEL: @test_mm512_mask_permutexvar_epi8
48 // CHECK: @llvm.x86.avx512.permvar.qi.512
49 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
50 return _mm512_mask_permutexvar_epi8(__W, __M, __A, __B);
51 }
52
test_mm512_mask_multishift_epi64_epi8(__m512i __W,__mmask64 __M,__m512i __X,__m512i __Y)53 __m512i test_mm512_mask_multishift_epi64_epi8(__m512i __W, __mmask64 __M, __m512i __X, __m512i __Y) {
54 // CHECK-LABEL: @test_mm512_mask_multishift_epi64_epi8
55 // CHECK: @llvm.x86.avx512.pmultishift.qb.512
56 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
57 return _mm512_mask_multishift_epi64_epi8(__W, __M, __X, __Y);
58 }
59
test_mm512_maskz_multishift_epi64_epi8(__mmask64 __M,__m512i __X,__m512i __Y)60 __m512i test_mm512_maskz_multishift_epi64_epi8(__mmask64 __M, __m512i __X, __m512i __Y) {
61 // CHECK-LABEL: @test_mm512_maskz_multishift_epi64_epi8
62 // CHECK: @llvm.x86.avx512.pmultishift.qb.512
63 // CHECK: select <64 x i1> %{{.*}}, <64 x i8> %{{.*}}, <64 x i8> %{{.*}}
64 return _mm512_maskz_multishift_epi64_epi8(__M, __X, __Y);
65 }
66
test_mm512_multishift_epi64_epi8(__m512i __X,__m512i __Y)67 __m512i test_mm512_multishift_epi64_epi8(__m512i __X, __m512i __Y) {
68 // CHECK-LABEL: @test_mm512_multishift_epi64_epi8
69 // CHECK: @llvm.x86.avx512.pmultishift.qb.512
70 return _mm512_multishift_epi64_epi8(__X, __Y);
71 }
72