1 // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512pf -emit-llvm -o - -Wall -Werror | FileCheck %s
2
3
4 #include <immintrin.h>
5
test_mm512_mask_prefetch_i32gather_pd(__m256i index,__mmask8 mask,void const * addr,int hint)6 void test_mm512_mask_prefetch_i32gather_pd(__m256i index, __mmask8 mask, void const *addr, int hint) {
7 // CHECK-LABEL: @test_mm512_mask_prefetch_i32gather_pd
8 // CHECK: @llvm.x86.avx512.gatherpf.dpd
9 return _mm512_mask_prefetch_i32gather_pd(index, mask, addr, 2, _MM_HINT_T0);
10 }
11
test_mm512_prefetch_i32gather_pd(__m256i index,void const * addr,int hint)12 void test_mm512_prefetch_i32gather_pd(__m256i index, void const *addr, int hint) {
13 // CHECK-LABEL: @test_mm512_prefetch_i32gather_pd
14 // CHECK: @llvm.x86.avx512.gatherpf.dpd
15 return _mm512_prefetch_i32gather_pd(index, addr, 2, _MM_HINT_T0);
16 }
17
test_mm512_mask_prefetch_i32gather_ps(__m512i index,__mmask16 mask,void const * addr,int hint)18 void test_mm512_mask_prefetch_i32gather_ps(__m512i index, __mmask16 mask, void const *addr, int hint) {
19 // CHECK-LABEL: @test_mm512_mask_prefetch_i32gather_ps
20 // CHECK: @llvm.x86.avx512.gatherpf.dps
21 return _mm512_mask_prefetch_i32gather_ps(index, mask, addr, 2, _MM_HINT_T0);
22 }
23
test_mm512_prefetch_i32gather_ps(__m512i index,void const * addr,int hint)24 void test_mm512_prefetch_i32gather_ps(__m512i index, void const *addr, int hint) {
25 // CHECK-LABEL: @test_mm512_prefetch_i32gather_ps
26 // CHECK: @llvm.x86.avx512.gatherpf.dps
27 return _mm512_prefetch_i32gather_ps(index, addr, 2, _MM_HINT_T0);
28 }
29
test_mm512_mask_prefetch_i64gather_pd(__m512i index,__mmask8 mask,void const * addr,int hint)30 void test_mm512_mask_prefetch_i64gather_pd(__m512i index, __mmask8 mask, void const *addr, int hint) {
31 // CHECK-LABEL: @test_mm512_mask_prefetch_i64gather_pd
32 // CHECK: @llvm.x86.avx512.gatherpf.qpd
33 return _mm512_mask_prefetch_i64gather_pd(index, mask, addr, 2, _MM_HINT_T0);
34 }
35
test_mm512_prefetch_i64gather_pd(__m512i index,void const * addr,int hint)36 void test_mm512_prefetch_i64gather_pd(__m512i index, void const *addr, int hint) {
37 // CHECK-LABEL: @test_mm512_prefetch_i64gather_pd
38 // CHECK: @llvm.x86.avx512.gatherpf.qpd
39 return _mm512_prefetch_i64gather_pd(index, addr, 2, _MM_HINT_T0);
40 }
41
test_mm512_mask_prefetch_i64gather_ps(__m512i index,__mmask8 mask,void const * addr,int hint)42 void test_mm512_mask_prefetch_i64gather_ps(__m512i index, __mmask8 mask, void const *addr, int hint) {
43 // CHECK-LABEL: @test_mm512_mask_prefetch_i64gather_ps
44 // CHECK: @llvm.x86.avx512.gatherpf.qps
45 return _mm512_mask_prefetch_i64gather_ps(index, mask, addr, 2, _MM_HINT_T0);
46 }
47
test_mm512_prefetch_i64gather_ps(__m512i index,void const * addr,int hint)48 void test_mm512_prefetch_i64gather_ps(__m512i index, void const *addr, int hint) {
49 // CHECK-LABEL: @test_mm512_prefetch_i64gather_ps
50 // CHECK: @llvm.x86.avx512.gatherpf.qps
51 return _mm512_prefetch_i64gather_ps(index, addr, 2, _MM_HINT_T0);
52 }
53
test_mm512_prefetch_i32scatter_pd(void * addr,__m256i index)54 void test_mm512_prefetch_i32scatter_pd(void *addr, __m256i index) {
55 // CHECK-LABEL: @test_mm512_prefetch_i32scatter_pd
56 // CHECK: @llvm.x86.avx512.scatterpf.dpd.512
57 return _mm512_prefetch_i32scatter_pd(addr, index, 1, _MM_HINT_T1);
58 }
59
test_mm512_mask_prefetch_i32scatter_pd(void * addr,__mmask8 mask,__m256i index)60 void test_mm512_mask_prefetch_i32scatter_pd(void *addr, __mmask8 mask, __m256i index) {
61 // CHECK-LABEL: @test_mm512_mask_prefetch_i32scatter_pd
62 // CHECK: @llvm.x86.avx512.scatterpf.dpd.512
63 return _mm512_mask_prefetch_i32scatter_pd(addr, mask, index, 1, _MM_HINT_T1);
64 }
65
test_mm512_prefetch_i32scatter_ps(void * addr,__m512i index)66 void test_mm512_prefetch_i32scatter_ps(void *addr, __m512i index) {
67 // CHECK-LABEL: @test_mm512_prefetch_i32scatter_ps
68 // CHECK: @llvm.x86.avx512.scatterpf.dps.512
69 return _mm512_prefetch_i32scatter_ps(addr, index, 1, _MM_HINT_T1);
70 }
71
test_mm512_mask_prefetch_i32scatter_ps(void * addr,__mmask16 mask,__m512i index)72 void test_mm512_mask_prefetch_i32scatter_ps(void *addr, __mmask16 mask, __m512i index) {
73 // CHECK-LABEL: @test_mm512_mask_prefetch_i32scatter_ps
74 // CHECK: @llvm.x86.avx512.scatterpf.dps.512
75 return _mm512_mask_prefetch_i32scatter_ps(addr, mask, index, 1, _MM_HINT_T1);
76 }
77
test_mm512_prefetch_i64scatter_pd(void * addr,__m512i index)78 void test_mm512_prefetch_i64scatter_pd(void *addr, __m512i index) {
79 // CHECK-LABEL: @test_mm512_prefetch_i64scatter_pd
80 // CHECK: @llvm.x86.avx512.scatterpf.qpd.512
81 return _mm512_prefetch_i64scatter_pd(addr, index, 1, _MM_HINT_T1);
82 }
83
test_mm512_mask_prefetch_i64scatter_pd(void * addr,__mmask16 mask,__m512i index)84 void test_mm512_mask_prefetch_i64scatter_pd(void *addr, __mmask16 mask, __m512i index) {
85 // CHECK-LABEL: @test_mm512_mask_prefetch_i64scatter_pd
86 // CHECK: @llvm.x86.avx512.scatterpf.qpd.512
87 return _mm512_mask_prefetch_i64scatter_pd(addr, mask, index, 1, _MM_HINT_T1);
88 }
89
test_mm512_prefetch_i64scatter_ps(void * addr,__m512i index)90 void test_mm512_prefetch_i64scatter_ps(void *addr, __m512i index) {
91 // CHECK-LABEL: @test_mm512_prefetch_i64scatter_ps
92 // CHECK: @llvm.x86.avx512.scatterpf.qps.512
93 return _mm512_prefetch_i64scatter_ps(addr, index, 1, _MM_HINT_T1);
94 }
95
test_mm512_mask_prefetch_i64scatter_ps(void * addr,__mmask16 mask,__m512i index)96 void test_mm512_mask_prefetch_i64scatter_ps(void *addr, __mmask16 mask, __m512i index) {
97 // CHECK-LABEL: @test_mm512_mask_prefetch_i64scatter_ps
98 // CHECK: @llvm.x86.avx512.scatterpf.qps.512
99 return _mm512_mask_prefetch_i64scatter_ps(addr, mask, index, 1, _MM_HINT_T1);
100 }
101