1 | // RUN: %clang_cc1 -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vbmi -emit-llvm -o - -Wall -Werror | FileCheck %s |
2 | |
3 | |
4 | #include <immintrin.h> |
5 | |
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 | |
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 | |
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 | |
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 | |
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 | |
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 | |
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 | |
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 | |
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 | |
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 | |