1 // RUN: %clang_cc1 -triple=x86_64-apple-darwin -fsyntax-only -verify %s
3 typedef long long __m128i
__attribute__((__vector_size__(16)));
4 typedef float __m128
__attribute__((__vector_size__(16)));
5 typedef double __m128d
__attribute__((__vector_size__(16)));
7 typedef long long __m256i
__attribute__((__vector_size__(32)));
8 typedef float __m256
__attribute__((__vector_size__(32)));
9 typedef double __m256d
__attribute__((__vector_size__(32)));
11 typedef long long __m512i
__attribute__((__vector_size__(64)));
12 typedef float __m512
__attribute__((__vector_size__(64)));
13 typedef double __m512d
__attribute__((__vector_size__(64)));
15 typedef unsigned char __mmask8
;
16 typedef unsigned short __mmask16
;
17 typedef unsigned int __mmask32
;
19 void call_x86_32_builtins(void) {
20 (void)__builtin_ia32_readeflags_u32(); // expected-error{{this builtin is only available on 32-bit targets}}
21 (void)__builtin_ia32_writeeflags_u32(4); // expected-error{{this builtin is only available on 32-bit targets}}
24 __m128
test__builtin_ia32_cmpps(__m128 __a
, __m128 __b
) {
25 return __builtin_ia32_cmpps(__a
, __b
, 32); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
28 __m128d
test__builtin_ia32_cmppd(__m128d __a
, __m128d __b
) {
29 return __builtin_ia32_cmppd(__a
, __b
, 32); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
32 __m128
test__builtin_ia32_cmpss(__m128 __a
, __m128 __b
) {
33 return __builtin_ia32_cmpss(__a
, __b
, 32); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
36 __m128d
test__builtin_ia32_cmpsd(__m128d __a
, __m128d __b
) {
37 return __builtin_ia32_cmpsd(__a
, __b
, 32); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
40 __mmask16
test__builtin_ia32_cmpps512_mask(__m512 __a
, __m512 __b
) {
41 return __builtin_ia32_cmpps512_mask(__a
, __b
, 32, -1, 4); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
44 __mmask8
test__builtin_ia32_cmppd512_mask(__m512d __a
, __m512d __b
) {
45 return __builtin_ia32_cmppd512_mask(__a
, __b
, 32, -1, 4); // expected-error {{argument value 32 is outside the valid range [0, 31]}}
48 __m128i
test__builtin_ia32_vpcomub(__m128i __a
, __m128i __b
) {
49 return __builtin_ia32_vpcomub(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
52 __m128i
test__builtin_ia32_vpcomuw(__m128i __a
, __m128i __b
) {
53 return __builtin_ia32_vpcomuw(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
56 __m128i
test__builtin_ia32_vpcomud(__m128i __a
, __m128i __b
) {
57 return __builtin_ia32_vpcomud(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
60 __m128i
test__builtin_ia32_vpcomuq(__m128i __a
, __m128i __b
) {
61 return __builtin_ia32_vpcomuq(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
64 __m128i
test__builtin_ia32_vpcomb(__m128i __a
, __m128i __b
) {
65 return __builtin_ia32_vpcomub(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
68 __m128i
test__builtin_ia32_vpcomw(__m128i __a
, __m128i __b
) {
69 return __builtin_ia32_vpcomuw(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
72 __m128i
test__builtin_ia32_vpcomd(__m128i __a
, __m128i __b
) {
73 return __builtin_ia32_vpcomud(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
76 __m128i
test__builtin_ia32_vpcomq(__m128i __a
, __m128i __b
) {
77 return __builtin_ia32_vpcomuq(__a
, __b
, 8); // expected-error {{argument value 8 is outside the valid range [0, 7]}}
80 __mmask16
test__builtin_ia32_cmpps512_mask_rounding(__m512 __a
, __m512 __b
, __mmask16 __u
) {
81 return __builtin_ia32_cmpps512_mask(__a
, __b
, 0, __u
, 0); // expected-error {{invalid rounding argument}}
84 // Make sure we allow 4(CUR_DIRECTION), 8(NO_EXC), and 12(CUR_DIRECTION|NOEXC) for SAE arguments.
85 __mmask16
test__builtin_ia32_cmpps512_mask_rounding_cur_dir(__m512 __a
, __m512 __b
, __mmask16 __u
) {
86 return __builtin_ia32_cmpps512_mask(__a
, __b
, 0, __u
, 4); // no-error
89 __mmask16
test__builtin_ia32_cmpps512_mask_rounding_sae1(__m512 __a
, __m512 __b
, __mmask16 __u
) {
90 return __builtin_ia32_cmpps512_mask(__a
, __b
, 0, __u
, 8); // no-error
93 __mmask16
test__builtin_ia32_cmpps512_mask_rounding_sae2(__m512 __a
, __m512 __b
, __mmask16 __u
) {
94 return __builtin_ia32_cmpps512_mask(__a
, __b
, 0, __u
, 12); // no-error
97 __m512
test__builtin_ia32_getmantps512_mask(__m512 a
, __m512 b
) {
98 return __builtin_ia32_getmantps512_mask(a
, 0, b
, (__mmask16
)-1, 10); // expected-error {{invalid rounding argument}}
101 __m128
test__builtin_ia32_getmantss_round_mask(__m128 a
, __m128 b
, __m128 c
) {
102 return __builtin_ia32_getmantss_round_mask(a
, b
, 0, c
, (__mmask8
)-1, 10); // expected-error {{invalid rounding argument}}
105 __m128i
test_mm_mask_i32gather_epi32(__m128i a
, int const *b
, __m128i c
, __m128i mask
) {
106 return __builtin_ia32_gatherd_d(a
, b
, c
, mask
, 5); // expected-error {{scale argument must be 1, 2, 4, or 8}}
109 void _mm512_mask_prefetch_i32gather_ps(__m512i index
, __mmask16 mask
, int const *addr
) {
110 __builtin_ia32_gatherpfdps(mask
, index
, addr
, 5, 1); // expected-error {{scale argument must be 1, 2, 4, or 8}}
113 void _mm512_mask_prefetch_i32gather_ps_2(__m512i index
, __mmask16 mask
, int const *addr
) {
114 __builtin_ia32_gatherpfdps(mask
, index
, addr
, 1, 1); // expected-error {{argument value 1 is outside the valid range [2, 3]}}
117 __m512i
test_mm512_shldi_epi64(__m512i __A
, __m512i __B
) {
118 return __builtin_ia32_vpshldq512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
121 __m512i
test_mm512_shldi_epi32(__m512i __A
, __m512i __B
) {
122 return __builtin_ia32_vpshldd512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
125 __m512i
test_mm512_shldi_epi16(__m512i __A
, __m512i __B
) {
126 return __builtin_ia32_vpshldw512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
129 __m512i
test_mm512_shrdi_epi64(__m512i __A
, __m512i __B
) {
130 return __builtin_ia32_vpshrdq512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
133 __m512i
test_mm512_shrdi_epi32(__m512i __A
, __m512i __B
) {
134 return __builtin_ia32_vpshrdd512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
137 __m512i
test_mm512_shrdi_epi16(__m512i __A
, __m512i __B
) {
138 return __builtin_ia32_vpshrdw512(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
141 __m256i
test_mm256_shldi_epi64(__m256i __A
, __m256i __B
) {
142 return __builtin_ia32_vpshldq256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
145 __m128i
test_mm128_shldi_epi64( __m128i __A
, __m128i __B
) {
146 return __builtin_ia32_vpshldq128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
149 __m256i
test_mm256_shldi_epi32(__m256i __A
, __m256i __B
) {
150 return __builtin_ia32_vpshldd256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
153 __m128i
test_mm128_shldi_epi32(__m128i __A
, __m128i __B
) {
154 return __builtin_ia32_vpshldd128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
157 __m256i
test_mm256_shldi_epi16( __m256i __A
, __m256i __B
) {
158 return __builtin_ia32_vpshldw256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
161 __m128i
test_mm128_shldi_epi16(__m128i __A
, __m128i __B
) {
162 return __builtin_ia32_vpshldw128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
165 __m256i
test_mm256_shrdi_epi64(__m256i __A
, __m256i __B
) {
166 return __builtin_ia32_vpshrdq256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
169 __m128i
test_mm128_shrdi_epi64(__m128i __A
, __m128i __B
) {
170 return __builtin_ia32_vpshrdq128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
173 __m256i
test_mm256_shrdi_epi32(__m256i __A
, __m256i __B
) {
174 return __builtin_ia32_vpshrdd256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
177 __m128i
test_mm128_shrdi_epi32(__m128i __A
, __m128i __B
) {
178 return __builtin_ia32_vpshrdd128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
181 __m256i
test_mm256_shrdi_epi16(__m256i __A
, __m256i __B
) {
182 return __builtin_ia32_vpshrdw256(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
185 __m128i
test_mm128_shrdi_epi16(__m128i __A
, __m128i __B
) {
186 return __builtin_ia32_vpshrdw128(__A
, __B
, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}
189 unsigned char test_lwpins32(unsigned int data2
, unsigned int data1
, unsigned int flags
) {
190 return __builtin_ia32_lwpins32(data2
, data1
, flags
); // expected-error {{argument to '__builtin_ia32_lwpins32' must be a constant integer}}
193 void test_lwpval32(unsigned int data2
, unsigned int data1
, unsigned int flags
) {
194 __builtin_ia32_lwpval32(data2
, data1
, flags
); // expected-error {{argument to '__builtin_ia32_lwpval32' must be a constant integer}}
197 unsigned char test_lwpins64(unsigned long long data2
, unsigned long long data1
, unsigned int flags
) {
198 return __builtin_ia32_lwpins64(data2
, data1
, flags
); // expected-error {{argument to '__builtin_ia32_lwpins64' must be a constant integer}}
201 void test_lwpval64(unsigned long long data2
, unsigned long long data1
, unsigned int flags
) {
202 __builtin_ia32_lwpval64(data2
, data1
, flags
); // expected-error {{argument to '__builtin_ia32_lwpval64' must be a constant integer}}