| 1 | // RUN: %clang_cc1 -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vnni -emit-llvm -o - -Wall -Werror | FileCheck %s |
|---|
| 2 | |
|---|
| 3 | #include <immintrin.h> |
|---|
| 4 | |
|---|
| 5 | __m512i test_mm512_mask_dpbusd_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) { |
|---|
| 6 | // CHECK-LABEL: @test_mm512_mask_dpbusd_epi32 |
|---|
| 7 | // CHECK: @llvm.x86.avx512.vpdpbusd.512 |
|---|
| 8 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 9 | return _mm512_mask_dpbusd_epi32(__S, __U, __A, __B); |
|---|
| 10 | } |
|---|
| 11 | |
|---|
| 12 | __m512i test_mm512_maskz_dpbusd_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) { |
|---|
| 13 | // CHECK-LABEL: @test_mm512_maskz_dpbusd_epi32 |
|---|
| 14 | // CHECK: @llvm.x86.avx512.vpdpbusd.512 |
|---|
| 15 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 16 | return _mm512_maskz_dpbusd_epi32(__U, __S, __A, __B); |
|---|
| 17 | } |
|---|
| 18 | |
|---|
| 19 | __m512i test_mm512_dpbusd_epi32(__m512i __S, __m512i __A, __m512i __B) { |
|---|
| 20 | // CHECK-LABEL: @test_mm512_dpbusd_epi32 |
|---|
| 21 | // CHECK: @llvm.x86.avx512.vpdpbusd.512 |
|---|
| 22 | return _mm512_dpbusd_epi32(__S, __A, __B); |
|---|
| 23 | } |
|---|
| 24 | |
|---|
| 25 | __m512i test_mm512_mask_dpbusds_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) { |
|---|
| 26 | // CHECK-LABEL: @test_mm512_mask_dpbusds_epi32 |
|---|
| 27 | // CHECK: @llvm.x86.avx512.vpdpbusds.51 |
|---|
| 28 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 29 | return _mm512_mask_dpbusds_epi32(__S, __U, __A, __B); |
|---|
| 30 | } |
|---|
| 31 | |
|---|
| 32 | __m512i test_mm512_maskz_dpbusds_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) { |
|---|
| 33 | // CHECK-LABEL: @test_mm512_maskz_dpbusds_epi32 |
|---|
| 34 | // CHECK: @llvm.x86.avx512.vpdpbusds.512 |
|---|
| 35 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 36 | return _mm512_maskz_dpbusds_epi32(__U, __S, __A, __B); |
|---|
| 37 | } |
|---|
| 38 | |
|---|
| 39 | __m512i test_mm512_dpbusds_epi32(__m512i __S, __m512i __A, __m512i __B) { |
|---|
| 40 | // CHECK-LABEL: @test_mm512_dpbusds_epi32 |
|---|
| 41 | // CHECK: @llvm.x86.avx512.vpdpbusds.512 |
|---|
| 42 | return _mm512_dpbusds_epi32(__S, __A, __B); |
|---|
| 43 | } |
|---|
| 44 | |
|---|
| 45 | __m512i test_mm512_mask_dpwssd_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) { |
|---|
| 46 | // CHECK-LABEL: @test_mm512_mask_dpwssd_epi32 |
|---|
| 47 | // CHECK: @llvm.x86.avx512.vpdpwssd.512 |
|---|
| 48 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 49 | return _mm512_mask_dpwssd_epi32(__S, __U, __A, __B); |
|---|
| 50 | } |
|---|
| 51 | |
|---|
| 52 | __m512i test_mm512_maskz_dpwssd_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) { |
|---|
| 53 | // CHECK-LABEL: @test_mm512_maskz_dpwssd_epi32 |
|---|
| 54 | // CHECK: @llvm.x86.avx512.vpdpwssd.512 |
|---|
| 55 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 56 | return _mm512_maskz_dpwssd_epi32(__U, __S, __A, __B); |
|---|
| 57 | } |
|---|
| 58 | |
|---|
| 59 | __m512i test_mm512_dpwssd_epi32(__m512i __S, __m512i __A, __m512i __B) { |
|---|
| 60 | // CHECK-LABEL: @test_mm512_dpwssd_epi32 |
|---|
| 61 | // CHECK: @llvm.x86.avx512.vpdpwssd.512 |
|---|
| 62 | return _mm512_dpwssd_epi32(__S, __A, __B); |
|---|
| 63 | } |
|---|
| 64 | |
|---|
| 65 | __m512i test_mm512_mask_dpwssds_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) { |
|---|
| 66 | // CHECK-LABEL: @test_mm512_mask_dpwssds_epi32 |
|---|
| 67 | // CHECK: @llvm.x86.avx512.vpdpwssds.512 |
|---|
| 68 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 69 | return _mm512_mask_dpwssds_epi32(__S, __U, __A, __B); |
|---|
| 70 | } |
|---|
| 71 | |
|---|
| 72 | __m512i test_mm512_maskz_dpwssds_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) { |
|---|
| 73 | // CHECK-LABEL: @test_mm512_maskz_dpwssds_epi32 |
|---|
| 74 | // CHECK: @llvm.x86.avx512.vpdpwssds.512 |
|---|
| 75 | // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}} |
|---|
| 76 | return _mm512_maskz_dpwssds_epi32(__U, __S, __A, __B); |
|---|
| 77 | } |
|---|
| 78 | |
|---|
| 79 | __m512i test_mm512_dpwssds_epi32(__m512i __S, __m512i __A, __m512i __B) { |
|---|
| 80 | // CHECK-LABEL: @test_mm512_dpwssds_epi32 |
|---|
| 81 | // CHECK: @llvm.x86.avx512.vpdpwssds.512 |
|---|
| 82 | return _mm512_dpwssds_epi32(__S, __A, __B); |
|---|
| 83 | } |
|---|
| 84 | |
|---|
| 85 | |
|---|