xref: /aosp_15_r20/external/clang/test/Headers/x86intrin-2.c (revision 67e74705e28f6214e480b399dd47ea732279e315)
1*67e74705SXin Li // RUN: %clang_cc1 -fsyntax-only -ffreestanding %s -verify
2*67e74705SXin Li // RUN: %clang_cc1 -fsyntax-only -ffreestanding -fno-lax-vector-conversions %s -verify
3*67e74705SXin Li // RUN: %clang_cc1 -fsyntax-only -ffreestanding -x c++ %s -verify
4*67e74705SXin Li // expected-no-diagnostics
5*67e74705SXin Li 
6*67e74705SXin Li #if defined(i386) || defined(__x86_64__)
7*67e74705SXin Li 
8*67e74705SXin Li // Include the metaheader that includes all x86 intrinsic headers.
9*67e74705SXin Li #include <x86intrin.h>
10*67e74705SXin Li 
mm_empty_wrap(void)11*67e74705SXin Li void __attribute__((__target__("mmx"))) mm_empty_wrap(void) {
12*67e74705SXin Li   _mm_empty();
13*67e74705SXin Li }
14*67e74705SXin Li 
mm_add_ss_wrap(__m128 a,__m128 b)15*67e74705SXin Li __m128 __attribute__((__target__("sse"))) mm_add_ss_wrap(__m128 a, __m128 b) {
16*67e74705SXin Li   return _mm_add_ss(a, b);
17*67e74705SXin Li }
18*67e74705SXin Li 
mm_sqrt_sd_wrap(__m128d a,__m128d b)19*67e74705SXin Li __m128d __attribute__((__target__("sse2"))) mm_sqrt_sd_wrap(__m128d a, __m128d b) {
20*67e74705SXin Li   return _mm_sqrt_sd(a, b);
21*67e74705SXin Li }
22*67e74705SXin Li 
mm_mwait_wrap(int a)23*67e74705SXin Li void __attribute__((__target__("sse3"))) mm_mwait_wrap(int a) {
24*67e74705SXin Li   _mm_mwait(0, 0);
25*67e74705SXin Li }
26*67e74705SXin Li 
mm_abs_pi8_wrap(__m64 a)27*67e74705SXin Li __m64 __attribute__((__target__("ssse3"))) mm_abs_pi8_wrap(__m64 a) {
28*67e74705SXin Li   return _mm_abs_pi8(a);
29*67e74705SXin Li }
30*67e74705SXin Li 
mm_minpos_epu16_wrap(__m128i v)31*67e74705SXin Li __m128i __attribute__((__target__("sse4.1"))) mm_minpos_epu16_wrap(__m128i v) {
32*67e74705SXin Li   return _mm_minpos_epu16(v);
33*67e74705SXin Li }
34*67e74705SXin Li 
mm_crc32_u8_wrap(unsigned int c,unsigned char d)35*67e74705SXin Li unsigned int __attribute__((__target__("sse4.2"))) mm_crc32_u8_wrap(unsigned int c, unsigned char d) {
36*67e74705SXin Li   return _mm_crc32_u8(c, d);
37*67e74705SXin Li }
38*67e74705SXin Li 
mm_aesenc_si128_wrap(__m128i v,__m128i r)39*67e74705SXin Li __m128i __attribute__((__target__("aes"))) mm_aesenc_si128_wrap(__m128i v, __m128i r) {
40*67e74705SXin Li   return _mm_aesenc_si128(v, r);
41*67e74705SXin Li }
42*67e74705SXin Li 
mm256_add_pd_wrap(__m256d a,__m256d b)43*67e74705SXin Li __m256d __attribute__((__target__("avx"))) mm256_add_pd_wrap(__m256d a, __m256d b) {
44*67e74705SXin Li   return _mm256_add_pd(a, b);
45*67e74705SXin Li }
46*67e74705SXin Li 
mm256_abs_epi8_wrap(__m256i a)47*67e74705SXin Li __m256i __attribute__((__target__("avx2"))) mm256_abs_epi8_wrap(__m256i a) {
48*67e74705SXin Li   return _mm256_abs_epi8(a);
49*67e74705SXin Li }
50*67e74705SXin Li 
tzcnt_u16_wrap(unsigned short x)51*67e74705SXin Li unsigned short __attribute__((__target__("bmi"))) tzcnt_u16_wrap(unsigned short x) {
52*67e74705SXin Li   return __tzcnt_u16(x);
53*67e74705SXin Li }
54*67e74705SXin Li 
bzhi_u32_wrap(unsigned int x,unsigned int y)55*67e74705SXin Li unsigned int __attribute__((__target__("bmi2"))) bzhi_u32_wrap(unsigned int x, unsigned int y) {
56*67e74705SXin Li   return _bzhi_u32(x, y);
57*67e74705SXin Li }
58*67e74705SXin Li 
lzcnt16_wrap(unsigned short x)59*67e74705SXin Li unsigned short __attribute__((__target__("lzcnt"))) lzcnt16_wrap(unsigned short x) {
60*67e74705SXin Li   return __lzcnt16(x);
61*67e74705SXin Li }
62*67e74705SXin Li 
mm256_fmsubadd_pd_wrap(__m256d a,__m256d b,__m256d c)63*67e74705SXin Li __m256d __attribute__((__target__("fma"))) mm256_fmsubadd_pd_wrap(__m256d a, __m256d b, __m256d c) {
64*67e74705SXin Li   return _mm256_fmsubadd_pd(a, b, c);
65*67e74705SXin Li }
66*67e74705SXin Li 
mm512_setzero_si512_wrap(void)67*67e74705SXin Li __m512i __attribute__((__target__("avx512f"))) mm512_setzero_si512_wrap(void) {
68*67e74705SXin Li   return _mm512_setzero_si512();
69*67e74705SXin Li }
70*67e74705SXin Li 
mm_cmpeq_epi32_mask_wrap(__m128i a,__m128i b)71*67e74705SXin Li __mmask8 __attribute__((__target__("avx512vl"))) mm_cmpeq_epi32_mask_wrap(__m128i a, __m128i b) {
72*67e74705SXin Li   return _mm_cmpeq_epi32_mask(a, b);
73*67e74705SXin Li }
74*67e74705SXin Li 
mm512_setzero_qi_wrap(void)75*67e74705SXin Li __m512i __attribute__((__target__("avx512bw"))) mm512_setzero_qi_wrap(void) {
76*67e74705SXin Li   return _mm512_setzero_qi();
77*67e74705SXin Li }
78*67e74705SXin Li 
mm512_mullo_epi64_wrap(__m512i a,__m512i b)79*67e74705SXin Li __m512i __attribute__((__target__("avx512dq"))) mm512_mullo_epi64_wrap(__m512i a, __m512i b) {
80*67e74705SXin Li   return _mm512_mullo_epi64(a, b);
81*67e74705SXin Li }
82*67e74705SXin Li 
mm_cmpeq_epi8_mask_wrap(__m128i a,__m128i b)83*67e74705SXin Li __mmask16 __attribute__((__target__("avx512vl,avx512bw"))) mm_cmpeq_epi8_mask_wrap(__m128i a, __m128i b) {
84*67e74705SXin Li   return _mm_cmpeq_epi8_mask(a, b);
85*67e74705SXin Li }
86*67e74705SXin Li 
mm256_mullo_epi64_wrap(__m256i a,__m256i b)87*67e74705SXin Li __m256i __attribute__((__target__("avx512vl,avx512dq"))) mm256_mullo_epi64_wrap(__m256i a, __m256i b) {
88*67e74705SXin Li   return _mm256_mullo_epi64(a, b);
89*67e74705SXin Li }
90*67e74705SXin Li 
rdrand16_step_wrap(unsigned short * p)91*67e74705SXin Li int __attribute__((__target__("rdrnd"))) rdrand16_step_wrap(unsigned short *p) {
92*67e74705SXin Li   return _rdrand16_step(p);
93*67e74705SXin Li }
94*67e74705SXin Li 
95*67e74705SXin Li #if defined(__x86_64__)
readfsbase_u32_wrap(void)96*67e74705SXin Li unsigned int __attribute__((__target__("fsgsbase"))) readfsbase_u32_wrap(void) {
97*67e74705SXin Li   return _readfsbase_u32();
98*67e74705SXin Li }
99*67e74705SXin Li #endif
100*67e74705SXin Li 
xbegin_wrap(void)101*67e74705SXin Li unsigned int __attribute__((__target__("rtm"))) xbegin_wrap(void) {
102*67e74705SXin Li   return _xbegin();
103*67e74705SXin Li }
104*67e74705SXin Li 
mm_sha1nexte_epu32_wrap(__m128i x,__m128i y)105*67e74705SXin Li __m128i __attribute__((__target__("sha"))) mm_sha1nexte_epu32_wrap(__m128i x, __m128i y) {
106*67e74705SXin Li   return _mm_sha1nexte_epu32(x, y);
107*67e74705SXin Li }
108*67e74705SXin Li 
rdseed16_step_wrap(unsigned short * p)109*67e74705SXin Li int __attribute__((__target__("rdseed"))) rdseed16_step_wrap(unsigned short *p) {
110*67e74705SXin Li   return _rdseed16_step(p);
111*67e74705SXin Li }
112*67e74705SXin Li 
mm_extract_si64_wrap(__m128i x,__m128i y)113*67e74705SXin Li __m128i __attribute__((__target__("sse4a"))) mm_extract_si64_wrap(__m128i x, __m128i y) {
114*67e74705SXin Li   return _mm_extract_si64(x, y);
115*67e74705SXin Li }
116*67e74705SXin Li 
mm_macc_ps_wrap(__m128 a,__m128 b,__m128 c)117*67e74705SXin Li __m128 __attribute__((__target__("fma4"))) mm_macc_ps_wrap(__m128 a, __m128 b, __m128 c) {
118*67e74705SXin Li   return _mm_macc_ps(a, b, c);
119*67e74705SXin Li }
120*67e74705SXin Li 
mm256_frcz_ps_wrap(__m256 a)121*67e74705SXin Li __m256 __attribute__((__target__("xop"))) mm256_frcz_ps_wrap(__m256 a) {
122*67e74705SXin Li   return _mm256_frcz_ps(a);
123*67e74705SXin Li }
124*67e74705SXin Li 
blcfill_u32_wrap(unsigned int a)125*67e74705SXin Li unsigned int __attribute__((__target__("tbm"))) blcfill_u32_wrap(unsigned int a) {
126*67e74705SXin Li   return __blcfill_u32(a);
127*67e74705SXin Li }
128*67e74705SXin Li 
mm_cvtph_ps_wrap(__m128i a)129*67e74705SXin Li __m128 __attribute__((__target__("f16c"))) mm_cvtph_ps_wrap(__m128i a) {
130*67e74705SXin Li   return _mm_cvtph_ps(a);
131*67e74705SXin Li }
132*67e74705SXin Li 
xtest_wrap(void)133*67e74705SXin Li int __attribute__((__target__("rtm"))) xtest_wrap(void) {
134*67e74705SXin Li   return _xtest();
135*67e74705SXin Li }
136*67e74705SXin Li 
137*67e74705SXin Li #endif
138