1 // RUN: %clang_cc1 %s -ffreestanding -triple=x86_64-unknown-unknown -target-feature +avxvnniint16 -emit-llvm -o - -Wall -Werror | FileCheck %s
2 // RUN: %clang_cc1 %s -ffreestanding -triple=i386-unknown-unknown -target-feature +avxvnniint16 -emit-llvm -o - -Wall -Werror | FileCheck %s
6 __m128i
test_mm_dpwsud_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
7 // CHECK-LABEL: @test_mm_dpwsud_epi32(
8 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwsud.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
9 return _mm_dpwsud_epi32(__A
, __B
, __C
);
12 __m256i
test_mm256_dpwsud_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
13 // CHECK-LABEL: @test_mm256_dpwsud_epi32(
14 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwsud.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
15 return _mm256_dpwsud_epi32(__A
, __B
, __C
);
18 __m128i
test_mm_dpwsuds_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
19 // CHECK-LABEL: @test_mm_dpwsuds_epi32(
20 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwsuds.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
21 return _mm_dpwsuds_epi32(__A
, __B
, __C
);
24 __m256i
test_mm256_dpwsuds_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
25 // CHECK-LABEL: @test_mm256_dpwsuds_epi32(
26 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwsuds.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
27 return _mm256_dpwsuds_epi32(__A
, __B
, __C
);
30 __m128i
test_mm_dpwusd_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
31 // CHECK-LABEL: @test_mm_dpwusd_epi32(
32 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwusd.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
33 return _mm_dpwusd_epi32(__A
, __B
, __C
);
36 __m256i
test_mm256_dpwusd_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
37 // CHECK-LABEL: @test_mm256_dpwusd_epi32(
38 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwusd.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
39 return _mm256_dpwusd_epi32(__A
, __B
, __C
);
42 __m128i
test_mm_dpwusds_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
43 // CHECK-LABEL: @test_mm_dpwusds_epi32(
44 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwusds.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
45 return _mm_dpwusds_epi32(__A
, __B
, __C
);
48 __m256i
test_mm256_dpwusds_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
49 // CHECK-LABEL: @test_mm256_dpwusds_epi32(
50 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwusds.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
51 return _mm256_dpwusds_epi32(__A
, __B
, __C
);
54 __m128i
test_mm_dpwuud_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
55 // CHECK-LABEL: @test_mm_dpwuud_epi32(
56 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwuud.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
57 return _mm_dpwuud_epi32(__A
, __B
, __C
);
60 __m256i
test_mm256_dpwuud_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
61 // CHECK-LABEL: @test_mm256_dpwuud_epi32(
62 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwuud.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
63 return _mm256_dpwuud_epi32(__A
, __B
, __C
);
66 __m128i
test_mm_dpwuuds_epi32(__m128i __A
, __m128i __B
, __m128i __C
) {
67 // CHECK-LABEL: @test_mm_dpwuuds_epi32(
68 // CHECK: call <4 x i32> @llvm.x86.avx2.vpdpwuuds.128(<4 x i32> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}})
69 return _mm_dpwuuds_epi32(__A
, __B
, __C
);
72 __m256i
test_mm256_dpwuuds_epi32(__m256i __A
, __m256i __B
, __m256i __C
) {
73 // CHECK-LABEL: @test_mm256_dpwuuds_epi32(
74 // CHECK: call <8 x i32> @llvm.x86.avx2.vpdpwuuds.256(<8 x i32> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}})
75 return _mm256_dpwuuds_epi32(__A
, __B
, __C
);