[clang] [Headers][X86] Add a couple of tests for MMX/SSE intrinsics (PR #105852)
Paul T Robinson via cfe-commits
cfe-commits at lists.llvm.org
Mon Aug 26 11:45:38 PDT 2024
https://github.com/pogo59 updated https://github.com/llvm/llvm-project/pull/105852
>From fbdf1c4a2bc88e1872bb6b91265b142319b7ccc8 Mon Sep 17 00:00:00 2001
From: Paul Robinson <paul.robinson at sony.com>
Date: Fri, 23 Aug 2024 09:40:08 -0700
Subject: [PATCH 1/2] [Headers][X86] Add a couple of tests for MMX/SSE
intrinsics
Certain intrinsics map to builtins that require an immediate (literal)
argument; make sure we report non-literal arguments.
Also verify that shift intrinsics map to the expected builtins.
These have been kicking around downstream for a while, and the recent
removal of the MMX builtins caused me to notice them again.
---
.../CodeGen/X86/mmx-sse2-shift-with-imm.c | 105 +++++
clang/test/Headers/x86-intrinsics-imm.c | 387 ++++++++++++++++++
2 files changed, 492 insertions(+)
create mode 100644 clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
create mode 100644 clang/test/Headers/x86-intrinsics-imm.c
diff --git a/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c b/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
new file mode 100644
index 00000000000000..3b386de50fa478
--- /dev/null
+++ b/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
@@ -0,0 +1,105 @@
+// RUN: %clang_cc1 -triple i386-unknown-unknown -target-feature +mmx \
+// RUN: -target-feature +sse2 -O0 -emit-llvm %s -o - | FileCheck %s
+
+// Test that mmx/sse2 shift intrinsics map to the expected builtins.
+
+// Don't include mm_malloc.h, it's system specific.
+#define __MM_MALLOC_H
+
+#include <x86intrin.h>
+
+__m64 check__mm_slli_pi16(__m64 m) {
+ // CHECK-LABEL: @check__mm_slli_pi16
+ // CHECK: @llvm.x86.sse2.pslli.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_slli_pi16(m, 8);
+}
+
+__m64 check__mm_slli_pi32(__m64 m) {
+ // CHECK-LABEL: @check__mm_slli_pi32
+ // CHECK: @llvm.x86.sse2.pslli.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_slli_pi32(m, 8);
+}
+
+__m64 check__mm_slli_si64(__m64 m) {
+ // CHECK-LABEL: @check__mm_slli_si64
+ // CHECK: @llvm.x86.sse2.pslli.q(<2 x i64> %{{.*}}, i32 {{.*}})
+ return _mm_slli_si64(m, 8);
+}
+
+__m64 check__mm_srai_pi16(__m64 m) {
+ // CHECK-LABEL: @check__mm_srai_pi16
+ // CHECK: @llvm.x86.sse2.psrai.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_srai_pi16(m, 8);
+}
+
+__m64 check__mm_srai_pi32(__m64 m) {
+ // CHECK-LABEL: @check__mm_srai_pi32
+ // CHECK: @llvm.x86.sse2.psrai.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_srai_pi32(m, 8);
+}
+
+__m64 check__mm_srli_pi16(__m64 m) {
+ // CHECK-LABEL: @check__mm_srli_pi16
+ // CHECK: @llvm.x86.sse2.psrli.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_srli_pi16(m, 8);
+}
+
+__m64 check__mm_srli_pi32(__m64 m) {
+ // CHECK-LABEL: @check__mm_srli_pi32
+ // CHECK: @llvm.x86.sse2.psrli.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_srli_pi32(m, 8);
+}
+
+__m64 check__mm_srli_si64(__m64 m) {
+ // CHECK-LABEL: @check__mm_srli_si64
+ // CHECK: @llvm.x86.sse2.psrli.q(<2 x i64> %{{.*}}, i32 {{.*}})
+ return _mm_srli_si64(m, 8);
+}
+
+__m128i check__mm_slli_epi16(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_slli_epi16
+ // CHECK: @llvm.x86.sse2.pslli.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_slli_epi16(a, b);
+}
+
+__m128i check__mm_slli_epi32(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_slli_epi32
+ // CHECK: @llvm.x86.sse2.pslli.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_slli_epi32(a, b);
+}
+
+__m128i check__mm_slli_epi64(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_slli_epi64
+ // CHECK: @llvm.x86.sse2.pslli.q(<2 x i64> %{{.*}}, i32 {{.*}})
+ return _mm_slli_epi64(a, b);
+}
+
+__m128i check__mm_srai_epi16(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_srai_epi16
+ // CHECK: @llvm.x86.sse2.psrai.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_srai_epi16(a, b);
+}
+
+__m128i check__mm_srai_epi32(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_srai_epi32
+ // CHECK: @llvm.x86.sse2.psrai.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_srai_epi32(a, b);
+}
+
+__m128i check__mm_srli_epi16(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_srli_epi16
+ // CHECK: @llvm.x86.sse2.psrli.w(<8 x i16> %{{.*}}, i32 {{.*}})
+ return _mm_srli_epi16(a, b);
+}
+
+__m128i check__mm_srli_epi32(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_srli_epi32
+ // CHECK: @llvm.x86.sse2.psrli.d(<4 x i32> %{{.*}}, i32 {{.*}})
+ return _mm_srli_epi32(a, b);
+}
+
+__m128i check__mm_srli_epi64(__m128i a, const int b) {
+ // CHECK-LABEL: @check__mm_srli_epi64
+ // CHECK: @llvm.x86.sse2.psrli.q(<2 x i64> %{{.*}}, i32 {{.*}})
+ return _mm_srli_epi64(a, b);
+}
diff --git a/clang/test/Headers/x86-intrinsics-imm.c b/clang/test/Headers/x86-intrinsics-imm.c
new file mode 100644
index 00000000000000..58bcf187b6f44f
--- /dev/null
+++ b/clang/test/Headers/x86-intrinsics-imm.c
@@ -0,0 +1,387 @@
+// RUN: %clang_cc1 -triple x86_64-unknown-unknown -fsyntax-only \
+// RUN: -target-feature +f16c -target-feature +avx -target-feature +sse4a \
+// RUN: -target-feature +aes -target-feature +xop -target-feature +avx2 \
+// RUN: -target-feature +tbm -verify %s
+
+// Error test cases where a variable is passed to intrinsics but an
+// immediate operand is required.
+
+// Don't include mm_malloc.h, it's system specific.
+#define __MM_MALLOC_H
+
+#include <x86intrin.h>
+
+unsigned short check__cvtss_sh(float val, const int I) {
+ return _cvtss_sh(val, I); // expected-error {{argument to '__builtin_ia32_vcvtps2ph' must be a constant integer}}
+}
+
+__m128i check__mm_cvtps_ph(__m128 val, const int I) {
+ return _mm_cvtps_ph(val, I); // expected-error {{argument to '__builtin_ia32_vcvtps2ph' must be a constant integer}}
+}
+
+__m128i check__mm256_cvtps_ph(__m256 val, const int I) {
+ return _mm256_cvtps_ph(val, I); // expected-error {{argument to '__builtin_ia32_vcvtps2ph256' must be a constant integer}}
+}
+
+// SCE_ARCH begin: bug 16381
+void check__mm_slli_si128(__m128i a, const int count) {
+ _mm_slli_si128(a, count); // expected-error {{argument to '__builtin_ia32_pslldqi128_byteshift' must be a constant integer}}
+}
+
+void check__mm_srli_si128(__m128i a, const int count) {
+ _mm_srli_si128(a, count); // expected-error {{argument to '__builtin_ia32_psrldqi128_byteshift' must be a constant integer}}
+}
+// SCE_ARCH end
+
+void check__mm_shuffle_epi32(__m128i a, const int imm) {
+ _mm_shuffle_epi32(a, imm); // expected-error {{argument to '__builtin_ia32_pshufd' must be a constant integer}}
+}
+
+void check__mm_shufflelo_epi16(__m128i a, const int imm) {
+ _mm_shufflelo_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshuflw' must be a constant integer}}
+}
+
+void check__mm_shufflehi_epi16(__m128i a, const int imm) {
+ _mm_shufflehi_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshufhw' must be a constant integer}}
+}
+
+void check__mm_shuffle_pd(__m128d a, __m128d b, const int i) {
+ _mm_shuffle_pd(a, b, i); // expected-error {{argument to '__builtin_ia32_shufpd' must be a constant integer}}
+}
+
+void check__mm256_round_pd(__m256d a, const int b) {
+ _mm256_round_pd(a, b); // expected-error {{argument to '__builtin_ia32_roundpd256' must be a constant integer}}
+}
+
+void check__mm256_round_ps(__m256 a, const int b) {
+ _mm256_round_ps(a, b); // expected-error {{argument to '__builtin_ia32_roundps256' must be a constant integer}}
+}
+
+void check__mm_permute_pd(__m128d a, const int b) {
+ _mm_permute_pd(a, b); // expected-error {{argument to '__builtin_ia32_vpermilpd' must be a constant integer}}
+}
+
+void check__mm256_permute_pd(__m256d a, const int b) {
+ _mm256_permute_pd(a, b); // expected-error {{argument to '__builtin_ia32_vpermilpd256' must be a constant integer}}
+}
+
+void check__mm_permute_ps(__m128 a, const int b) {
+ _mm_permute_ps(a, b); // expected-error {{argument to '__builtin_ia32_vpermilps' must be a constant integer}}
+}
+
+void check__mm256_permute_ps(__m256 a, const int b) {
+ _mm256_permute_ps(a, b); // expected-error {{argument to '__builtin_ia32_vpermilps256' must be a constant integer}}
+}
+
+void check__mm256_permute2f128_pd(__m256d v1, __m256d v2, const char m) {
+ _mm256_permute2f128_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_pd256' must be a constant integer}}
+}
+
+void check__mm256_permute2f128_ps(__m256 v1, __m256 v2, const char m) {
+ _mm256_permute2f128_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_ps256' must be a constant integer}}
+}
+
+void check__mm256_permute2f128_si256(__m256i v1, __m256i v2, const char m) {
+ _mm256_permute2f128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_si256' must be a constant integer}}
+}
+
+void check__m256_blend_pd(__m256d v1, __m256d v2, const char m) {
+ _mm256_blend_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendpd256' must be a constant integer}}
+}
+
+void check__m256_blend_ps(__m256 v1, __m256 v2, const char m) {
+ _mm256_blend_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendps256' must be a constant integer}}
+}
+
+void check__mm256_dp_ps(__m256 v1, __m256 v2, const char m) {
+ _mm256_dp_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_dpps256' must be a constant integer}}
+}
+
+void check__m256_shuffle_ps(__m256 a, __m256 b, const int m) {
+ _mm256_shuffle_ps(a, b, m); // expected-error {{argument to '__builtin_ia32_shufps256' must be a constant integer}}
+}
+
+void check__m256_shuffle_pd(__m256d a, __m256d b, const int m) {
+ _mm256_shuffle_pd(a, b, m); // expected-error {{argument to '__builtin_ia32_shufpd256' must be a constant integer}}
+}
+
+void check__mm_cmp_pd(__m128d a, __m128d b, const int c) {
+ _mm_cmp_pd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmppd' must be a constant integer}}
+}
+
+void check__mm_cmp_ps(__m128 a, __m128 b, const int c) {
+ _mm_cmp_ps(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpps' must be a constant integer}}
+}
+
+void check__mm256_cmp_pd(__m256d a, __m256d b, const int c) {
+ _mm256_cmp_pd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmppd256' must be a constant integer}}
+}
+
+void check__mm256_cmp_ps(__m256 a, __m256 b, const int c) {
+ _mm256_cmp_ps(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpps256' must be a constant integer}}
+}
+
+void check__mm_cmp_sd(__m128d a, __m128d b, const int c) {
+ _mm_cmp_sd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpsd' must be a constant integer}}
+}
+
+void check__mm_cmp_ss(__m128 a, __m128 b, const int c) {
+ _mm_cmp_ss(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpss' must be a constant integer}}
+}
+
+void check__mm256_extractf128_pd(__m256d a, const int o) {
+ _mm256_extractf128_pd(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_pd256' must be a constant integer}}
+}
+
+void check__mm256_extractf128_ps(__m256 a, const int o) {
+ _mm256_extractf128_ps(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_ps256' must be a constant integer}}
+}
+
+void check__mm256_extractf128_si256(__m256i a, const int o) {
+ _mm256_extractf128_si256(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_si256' must be a constant integer}}
+}
+
+void check__mm256_insertf128_pd(__m256d v1, __m128d v2, const int o) {
+ _mm256_insertf128_pd(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_pd256' must be a constant integer}}
+}
+
+void check__mm256_insertf128_ps(__m256 v1, __m128 v2, const int o) {
+ _mm256_insertf128_ps(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_ps256' must be a constant integer}}
+}
+
+void check__mm256_insertf128_si256(__m256i v1, __m128i v2, const int o) {
+ _mm256_insertf128_si256(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_si256' must be a constant integer}}
+}
+
+void check__mm_round_ps(__m128 x, const int m) {
+ _mm_round_ps(x, m); // expected-error {{argument to '__builtin_ia32_roundps' must be a constant integer}}
+}
+
+void check__mm_round_ss(__m128 x, __m128 y, const int m) {
+ _mm_round_ss(x, y, m); // expected-error {{argument to '__builtin_ia32_roundss' must be a constant integer}}
+}
+
+void check__mm_round_pd(__m128d x, const int m) {
+ _mm_round_pd(x, m); // expected-error {{argument to '__builtin_ia32_roundpd' must be a constant integer}}
+}
+
+void check__mm_round_sd(__m128d x, __m128d y, const int m) {
+ _mm_round_sd(x, y, m); // expected-error {{argument to '__builtin_ia32_roundsd' must be a constant integer}}
+}
+
+void check__mm_blend_pd(__m128d v1, __m128d v2, const int m) {
+ _mm_blend_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendpd' must be a constant integer}}
+}
+
+void check__mm_blend_ps(__m128 v1, __m128 v2, const int m) {
+ _mm_blend_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendps' must be a constant integer}}
+}
+
+void check__mm_blend_epi16(__m128i v1, __m128i v2, const int m) {
+ _mm_blend_epi16(v1, v2, m); // expected-error {{argument to '__builtin_ia32_pblendw128' must be a constant integer}}
+}
+
+void check__mm_dp_ps(__m128 x, __m128 y, const int m) {
+ _mm_dp_ps(x, y, m); // expected-error {{argument to '__builtin_ia32_dpps' must be a constant integer}}
+}
+
+void check__mm_dp_pd(__m128d x, __m128d y, const int m) {
+ _mm_dp_pd(x, y, m); // expected-error {{argument to '__builtin_ia32_dppd' must be a constant integer}}
+}
+
+void check__mm_insert_ps(__m128 a, __m128 b, const int n) {
+ _mm_insert_ps(a, b, n); // expected-error {{argument to '__builtin_ia32_insertps128' must be a constant integer}}
+}
+
+void check__mm_mpsadbw_epu8(__m128i x, __m128i y, const int m) {
+ _mm_mpsadbw_epu8(x, y, m); // expected-error {{argument to '__builtin_ia32_mpsadbw128' must be a constant integer}}
+}
+
+void check__mm_cmpistrm(__m128 a, __m128 b, const int m) {
+ _mm_cmpistrm(a, b, m); // expected-error {{argument to '__builtin_ia32_pcmpistrm128' must be a constant integer}}
+}
+
+void check__mm_cmpistri(__m128i a, __m128i b, const int m) {
+ _mm_cmpistri(a, b, m); // expected-error {{argument to '__builtin_ia32_pcmpistri128' must be a constant integer}}
+}
+
+void check__mm_cmpestrm(__m128 a, int b, __m128 c, int d, const int m) {
+ _mm_cmpestrm(a, b, c, d, m); // expected-error {{argument to '__builtin_ia32_pcmpestrm128' must be a constant integer}}
+}
+
+void check__mm_cmpestri(__m128i a, int b, __m128i c, int d, const int m) {
+ _mm_cmpestri(a, b, c, d, m); // expected-error {{argument to '__builtin_ia32_pcmpestri128' must be a constant integer}}
+}
+
+void check__mm_alignr_epi8(__m128i a, __m128i b, const int n) {
+ _mm_alignr_epi8(a, b, n); // expected-error {{argument to '__builtin_ia32_palignr128' must be a constant integer}}
+}
+
+void check__mm_alignr_pi8(__m64 a, __m64 b, const int n) {
+ _mm_alignr_pi8(a, b, n); // expected-error {{argument to '__builtin_ia32_psrldqi128_byteshift' must be a constant integer}}
+}
+
+void check__mm_aeskeygenassist_si128(__m128 c, const int r) {
+ _mm_aeskeygenassist_si128(c, r); // expected-error {{argument to '__builtin_ia32_aeskeygenassist128' must be a constant integer}}
+}
+
+__m64 check__mm_shuffle_pi16(__m64 a, const int n) {
+ return _mm_shuffle_pi16(a, n); // expected-error {{index for __builtin_shufflevector must be a constant integer}}
+}
+
+void check__mm_shuffle_ps(__m128 a, __m128 b, const int m) {
+ _mm_shuffle_ps(a, b, m); // expected-error {{argument to '__builtin_ia32_shufps' must be a constant integer}}
+}
+
+void check__mm_com_epi8(__m128 a, __m128 b, const char c) {
+ _mm_com_epi8(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomb' must be a constant integer}}
+}
+
+void check__mm_com_epi16(__m128 a, __m128 b, const char c) {
+ _mm_com_epi16(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomw' must be a constant integer}}
+}
+
+void check__mm_com_epi32(__m128 a, __m128 b, const char c) {
+ _mm_com_epi32(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomd' must be a constant integer}}
+}
+
+void check__mm_com_epi64(__m128 a, __m128 b, const char c) {
+ _mm_com_epi64(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomq' must be a constant integer}}
+}
+
+void check__mm_com_epu8(__m128 a, __m128 b, const char c) {
+ _mm_com_epu8(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomub' must be a constant integer}}
+}
+
+void check__mm_com_epu16(__m128 a, __m128 b, const char c) {
+ _mm_com_epu16(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomuw' must be a constant integer}}
+}
+
+void check__mm_com_epu32(__m128 a, __m128 b, const char c) {
+ _mm_com_epu32(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomud' must be a constant integer}}
+}
+
+void check__mm_com_epu64(__m128 a, __m128 b, const char c) {
+ _mm_com_epu64(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomuq' must be a constant integer}}
+}
+
+void check__mm_permute2_pd(__m128d a, __m128d b, __m128d c, const char d) {
+ _mm_permute2_pd(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2pd' must be a constant integer}}
+}
+
+void check__mm_permute2_ps(__m128 a, __m128 b, __m128 c, const char d) {
+ _mm_permute2_ps(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2ps' must be a constant integer}}
+}
+
+void check__mm256_permute2_pd(__m256d a, __m256d b, __m256d c, const char d) {
+ _mm256_permute2_pd(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2pd256' must be a constant integer}}
+}
+
+void check__mm256_permute2_ps(__m256 a, __m256 b, __m256 c, const char d) {
+ _mm256_permute2_ps(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2ps256' must be a constant integer}}
+}
+
+void check__mm_roti_epi8(__m128 a, const char b) {
+ _mm_roti_epi8(a, b); // expected-error {{argument to '__builtin_ia32_vprotbi' must be a constant integer}}
+}
+
+void check__mm_roti_epi16(__m128 a, const char b) {
+ _mm_roti_epi16(a, b); // expected-error {{argument to '__builtin_ia32_vprotwi' must be a constant integer}}
+}
+
+void check__mm_roti_epi32(__m128 a, const char b) {
+ _mm_roti_epi32(a, b); // expected-error {{argument to '__builtin_ia32_vprotdi' must be a constant integer}}
+}
+
+void check__mm_roti_epi64(__m128 a, const char b) {
+ _mm_roti_epi64(a, b); // expected-error {{argument to '__builtin_ia32_vprotqi' must be a constant integer}}
+}
+
+void check__mm256_mpsadbw_epu8(__m256i a, __m256i b, const int c) {
+ _mm256_mpsadbw_epu8(a, b, c); // expected-error {{argument to '__builtin_ia32_mpsadbw256' must be a constant integer}}
+}
+
+void check__mm256_alignr_epi8(__m256i a, __m256i b, const int n) {
+ _mm256_alignr_epi8(a, b, n); // expected-error {{argument to '__builtin_ia32_palignr256' must be a constant integer}}
+}
+
+void check__mm256_blend_epi16(__m256i a, __m256i b, const int m) {
+ _mm256_blend_epi16(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendw256' must be a constant integer}}
+}
+
+void check__mm256_slli_si256(__m256i a, const int count) {
+ _mm256_slli_si256(a, count); // expected-error {{argument to '__builtin_ia32_pslldqi256_byteshift' must be a constant integer}}
+}
+
+void check__mm256_shuffle_epi32(__m256i a, const int imm) {
+ _mm256_shuffle_epi32(a, imm); // expected-error {{argument to '__builtin_ia32_pshufd256' must be a constant integer}}
+}
+
+void check__mm256_shufflehi_epi16(__m256i a, const int imm) {
+ _mm256_shufflehi_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshufhw256' must be a constant integer}}
+}
+
+void check__mm256_shufflelo_epi16(__m256i a, const int imm) {
+ _mm256_shufflelo_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshuflw256' must be a constant integer}}
+}
+
+void check__mm_blend_epi32(__m128i a, __m128i b, const int m) {
+ _mm_blend_epi32(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendd128' must be a constant integer}}
+}
+
+void check__mm256_blend_epi32(__m256i a, __m256i b, const int m) {
+ _mm256_blend_epi32(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendd256' must be a constant integer}}
+}
+
+void check__mm256_permute4x64_pd(__m256d v, const int m) {
+ _mm256_permute4x64_pd(v, m); // expected-error {{argument to '__builtin_ia32_permdf256' must be a constant integer}}
+}
+
+void check__mm256_permute4x64_epi64(__m256i v, const int m) {
+ _mm256_permute4x64_epi64(v, m); // expected-error {{argument to '__builtin_ia32_permdi256' must be a constant integer}}
+}
+
+void check__mm256_permute2x128_si256(__m256i v1, __m256i v2, const int m) {
+ _mm256_permute2x128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_permti256' must be a constant integer}}
+}
+
+void check__mm256_extracti128_si256(__m256i v1, const int m) {
+ _mm256_extracti128_si256(v1, m); // expected-error {{argument to '__builtin_ia32_extract128i256' must be a constant integer}}
+}
+
+void check__mm256_inserti128_si256(__m256i v1, __m128i v2, const int m) {
+ _mm256_inserti128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_insert128i256' must be a constant integer}}
+}
+
+void check__mm256_srli_si256(__m256i a, int count) {
+ _mm256_srli_si256(a, count); // expected-error {{argument to '__builtin_ia32_psrldqi256_byteshift' must be a constant integer}}
+}
+
+int check__bextri_u32(int a, int b) {
+ return __bextri_u32(a, b); // expected-error {{argument to '__builtin_ia32_bextri_u32' must be a constant integer}}
+}
+
+int check__bextri_u64(long a, long b) {
+ return __bextri_u64(a, b); // expected-error {{argument to '__builtin_ia32_bextri_u64' must be a constant integer}}
+}
+
+int check___builtin_eh_return_data_regno(int a) {
+ return __builtin_eh_return_data_regno(a); // expected-error {{argument to '__builtin_eh_return_data_regno' must be a constant integer}}
+}
+
+void* check___builtin_frame_address(unsigned int a) {
+ return __builtin_frame_address(a); // expected-error {{argument to '__builtin_frame_address' must be a constant integer}}
+}
+
+void* check___builtin_return_address(unsigned int a) {
+ return __builtin_return_address(a); // expected-error {{argument to '__builtin_return_address' must be a constant integer}}
+}
+
+void check__mm_extracti_si64(__m128i a, const char len, const char id) {
+ _mm_extracti_si64(a, len, id); // expected-error {{argument to '__builtin_ia32_extrqi' must be a constant integer}}
+}
+
+void check__insert_si64(__m128 a, __m128 b, const char len, const char id) {
+ _mm_inserti_si64(a, b, len, id); // expected-error {{argument to '__builtin_ia32_insertqi' must be a constant integer}}
+}
+
>From 72b329605ecd6b12cb42e60c6243d71d29aa86b6 Mon Sep 17 00:00:00 2001
From: Paul Robinson <paul.robinson at sony.com>
Date: Mon, 26 Aug 2024 11:45:25 -0700
Subject: [PATCH 2/2] Update per review feedback
---
.../CodeGen/X86/mmx-sse2-shift-with-imm.c | 105 ------------------
.../X86}/x86-intrinsics-imm.c | 0
2 files changed, 105 deletions(-)
delete mode 100644 clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
rename clang/test/{Headers => CodeGen/X86}/x86-intrinsics-imm.c (100%)
diff --git a/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c b/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
deleted file mode 100644
index 3b386de50fa478..00000000000000
--- a/clang/test/CodeGen/X86/mmx-sse2-shift-with-imm.c
+++ /dev/null
@@ -1,105 +0,0 @@
-// RUN: %clang_cc1 -triple i386-unknown-unknown -target-feature +mmx \
-// RUN: -target-feature +sse2 -O0 -emit-llvm %s -o - | FileCheck %s
-
-// Test that mmx/sse2 shift intrinsics map to the expected builtins.
-
-// Don't include mm_malloc.h, it's system specific.
-#define __MM_MALLOC_H
-
-#include <x86intrin.h>
-
-__m64 check__mm_slli_pi16(__m64 m) {
- // CHECK-LABEL: @check__mm_slli_pi16
- // CHECK: @llvm.x86.sse2.pslli.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_slli_pi16(m, 8);
-}
-
-__m64 check__mm_slli_pi32(__m64 m) {
- // CHECK-LABEL: @check__mm_slli_pi32
- // CHECK: @llvm.x86.sse2.pslli.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_slli_pi32(m, 8);
-}
-
-__m64 check__mm_slli_si64(__m64 m) {
- // CHECK-LABEL: @check__mm_slli_si64
- // CHECK: @llvm.x86.sse2.pslli.q(<2 x i64> %{{.*}}, i32 {{.*}})
- return _mm_slli_si64(m, 8);
-}
-
-__m64 check__mm_srai_pi16(__m64 m) {
- // CHECK-LABEL: @check__mm_srai_pi16
- // CHECK: @llvm.x86.sse2.psrai.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_srai_pi16(m, 8);
-}
-
-__m64 check__mm_srai_pi32(__m64 m) {
- // CHECK-LABEL: @check__mm_srai_pi32
- // CHECK: @llvm.x86.sse2.psrai.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_srai_pi32(m, 8);
-}
-
-__m64 check__mm_srli_pi16(__m64 m) {
- // CHECK-LABEL: @check__mm_srli_pi16
- // CHECK: @llvm.x86.sse2.psrli.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_srli_pi16(m, 8);
-}
-
-__m64 check__mm_srli_pi32(__m64 m) {
- // CHECK-LABEL: @check__mm_srli_pi32
- // CHECK: @llvm.x86.sse2.psrli.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_srli_pi32(m, 8);
-}
-
-__m64 check__mm_srli_si64(__m64 m) {
- // CHECK-LABEL: @check__mm_srli_si64
- // CHECK: @llvm.x86.sse2.psrli.q(<2 x i64> %{{.*}}, i32 {{.*}})
- return _mm_srli_si64(m, 8);
-}
-
-__m128i check__mm_slli_epi16(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_slli_epi16
- // CHECK: @llvm.x86.sse2.pslli.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_slli_epi16(a, b);
-}
-
-__m128i check__mm_slli_epi32(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_slli_epi32
- // CHECK: @llvm.x86.sse2.pslli.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_slli_epi32(a, b);
-}
-
-__m128i check__mm_slli_epi64(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_slli_epi64
- // CHECK: @llvm.x86.sse2.pslli.q(<2 x i64> %{{.*}}, i32 {{.*}})
- return _mm_slli_epi64(a, b);
-}
-
-__m128i check__mm_srai_epi16(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_srai_epi16
- // CHECK: @llvm.x86.sse2.psrai.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_srai_epi16(a, b);
-}
-
-__m128i check__mm_srai_epi32(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_srai_epi32
- // CHECK: @llvm.x86.sse2.psrai.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_srai_epi32(a, b);
-}
-
-__m128i check__mm_srli_epi16(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_srli_epi16
- // CHECK: @llvm.x86.sse2.psrli.w(<8 x i16> %{{.*}}, i32 {{.*}})
- return _mm_srli_epi16(a, b);
-}
-
-__m128i check__mm_srli_epi32(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_srli_epi32
- // CHECK: @llvm.x86.sse2.psrli.d(<4 x i32> %{{.*}}, i32 {{.*}})
- return _mm_srli_epi32(a, b);
-}
-
-__m128i check__mm_srli_epi64(__m128i a, const int b) {
- // CHECK-LABEL: @check__mm_srli_epi64
- // CHECK: @llvm.x86.sse2.psrli.q(<2 x i64> %{{.*}}, i32 {{.*}})
- return _mm_srli_epi64(a, b);
-}
diff --git a/clang/test/Headers/x86-intrinsics-imm.c b/clang/test/CodeGen/X86/x86-intrinsics-imm.c
similarity index 100%
rename from clang/test/Headers/x86-intrinsics-imm.c
rename to clang/test/CodeGen/X86/x86-intrinsics-imm.c
More information about the cfe-commits
mailing list