Elad Cohen | b107a22 | 2016-09-28 11:59:09 +0000 | [diff] [blame] | 1 | // RUN: %clang_cc1 -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512pf -emit-llvm -o - -Wall -Werror | FileCheck %s |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 2 | |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 3 | |
| 4 | #include <immintrin.h> |
| 5 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 9 | return _mm512_mask_prefetch_i32gather_pd(index, mask, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 10 | } |
| 11 | |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 15 | return _mm512_prefetch_i32gather_pd(index, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 16 | } |
| 17 | |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 21 | return _mm512_mask_prefetch_i32gather_ps(index, mask, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 22 | } |
| 23 | |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 27 | return _mm512_prefetch_i32gather_ps(index, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 28 | } |
| 29 | |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 33 | return _mm512_mask_prefetch_i64gather_pd(index, mask, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 34 | } |
| 35 | |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 39 | return _mm512_prefetch_i64gather_pd(index, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 40 | } |
| 41 | |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 45 | return _mm512_mask_prefetch_i64gather_ps(index, mask, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | 4fa96af | 2016-04-21 12:47:27 +0000 | [diff] [blame] | 46 | } |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 47 | |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 51 | return _mm512_prefetch_i64gather_ps(index, addr, 2, _MM_HINT_T0); |
Michael Zuckerman | c49f6ce | 2016-06-14 13:45:17 +0000 | [diff] [blame] | 52 | } |
| 53 | |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 57 | return _mm512_prefetch_i32scatter_pd(addr, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 58 | } |
| 59 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 63 | return _mm512_mask_prefetch_i32scatter_pd(addr, mask, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 64 | } |
| 65 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 69 | return _mm512_prefetch_i32scatter_ps(addr, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 70 | } |
| 71 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 75 | return _mm512_mask_prefetch_i32scatter_ps(addr, mask, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 76 | } |
| 77 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 81 | return _mm512_prefetch_i64scatter_pd(addr, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 82 | } |
| 83 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 87 | return _mm512_mask_prefetch_i64scatter_pd(addr, mask, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 88 | } |
| 89 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 93 | return _mm512_prefetch_i64scatter_ps(addr, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 94 | } |
| 95 | |
| 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 |
Craig Topper | f771f79b | 2017-03-31 17:22:30 +0000 | [diff] [blame] | 99 | return _mm512_mask_prefetch_i64scatter_ps(addr, mask, index, 1, _MM_HINT_T1); |
Michael Zuckerman | fcf32c2 | 2016-04-25 13:01:40 +0000 | [diff] [blame] | 100 | } |