196 lines · c
1// RUN: %clang_cc1 -triple=x86_64-apple-darwin -fsyntax-only -verify %s2 3typedef long long __m128i __attribute__((__vector_size__(16)));4typedef float __m128 __attribute__((__vector_size__(16)));5typedef double __m128d __attribute__((__vector_size__(16)));6 7typedef long long __m256i __attribute__((__vector_size__(32)));8typedef float __m256 __attribute__((__vector_size__(32)));9typedef double __m256d __attribute__((__vector_size__(32)));10 11typedef long long __m512i __attribute__((__vector_size__(64)));12typedef float __m512 __attribute__((__vector_size__(64)));13typedef double __m512d __attribute__((__vector_size__(64)));14 15typedef unsigned char __mmask8;16typedef unsigned short __mmask16;17typedef unsigned int __mmask32;18 19void 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}}22}23 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]}}26}27 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]}}30}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]}}34}35 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]}}38}39 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]}}42}43 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]}}46}47 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]}}50}51 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]}}54}55 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]}}58}59 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]}}62}63 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]}}66}67 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]}}70}71 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]}}74}75 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]}}78}79 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}}82}83 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-error87}88 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-error91}92 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-error95}96 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}}99}100 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}}103}104 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}}107}108 109__m512i test_mm512_shldi_epi64(__m512i __A, __m512i __B) {110 return __builtin_ia32_vpshldq512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}111}112 113__m512i test_mm512_shldi_epi32(__m512i __A, __m512i __B) {114 return __builtin_ia32_vpshldd512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}115}116 117__m512i test_mm512_shldi_epi16(__m512i __A, __m512i __B) {118 return __builtin_ia32_vpshldw512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}119}120 121__m512i test_mm512_shrdi_epi64(__m512i __A, __m512i __B) {122 return __builtin_ia32_vpshrdq512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}123}124 125__m512i test_mm512_shrdi_epi32(__m512i __A, __m512i __B) {126 return __builtin_ia32_vpshrdd512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}127}128 129__m512i test_mm512_shrdi_epi16(__m512i __A, __m512i __B) {130 return __builtin_ia32_vpshrdw512(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}131}132 133__m256i test_mm256_shldi_epi64(__m256i __A, __m256i __B) {134 return __builtin_ia32_vpshldq256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}135}136 137__m128i test_mm128_shldi_epi64( __m128i __A, __m128i __B) {138 return __builtin_ia32_vpshldq128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}139}140 141__m256i test_mm256_shldi_epi32(__m256i __A, __m256i __B) {142 return __builtin_ia32_vpshldd256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}143}144 145__m128i test_mm128_shldi_epi32(__m128i __A, __m128i __B) {146 return __builtin_ia32_vpshldd128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}147}148 149__m256i test_mm256_shldi_epi16( __m256i __A, __m256i __B) {150 return __builtin_ia32_vpshldw256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}151}152 153__m128i test_mm128_shldi_epi16(__m128i __A, __m128i __B) {154 return __builtin_ia32_vpshldw128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}155}156 157__m256i test_mm256_shrdi_epi64(__m256i __A, __m256i __B) {158 return __builtin_ia32_vpshrdq256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}159}160 161__m128i test_mm128_shrdi_epi64(__m128i __A, __m128i __B) {162 return __builtin_ia32_vpshrdq128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}163}164 165__m256i test_mm256_shrdi_epi32(__m256i __A, __m256i __B) {166 return __builtin_ia32_vpshrdd256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}167}168 169__m128i test_mm128_shrdi_epi32(__m128i __A, __m128i __B) {170 return __builtin_ia32_vpshrdd128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}171}172 173__m256i test_mm256_shrdi_epi16(__m256i __A, __m256i __B) {174 return __builtin_ia32_vpshrdw256(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}175}176 177__m128i test_mm128_shrdi_epi16(__m128i __A, __m128i __B) {178 return __builtin_ia32_vpshrdw128(__A, __B, 1024); // expected-error {{argument value 1024 is outside the valid range [0, 255]}}179}180 181unsigned char test_lwpins32(unsigned int data2, unsigned int data1, unsigned int flags) {182 return __builtin_ia32_lwpins32(data2, data1, flags); // expected-error {{argument to '__builtin_ia32_lwpins32' must be a constant integer}}183}184 185void test_lwpval32(unsigned int data2, unsigned int data1, unsigned int flags) {186 __builtin_ia32_lwpval32(data2, data1, flags); // expected-error {{argument to '__builtin_ia32_lwpval32' must be a constant integer}}187}188 189unsigned char test_lwpins64(unsigned long long data2, unsigned long long data1, unsigned int flags) {190 return __builtin_ia32_lwpins64(data2, data1, flags); // expected-error {{argument to '__builtin_ia32_lwpins64' must be a constant integer}}191}192 193void test_lwpval64(unsigned long long data2, unsigned long long data1, unsigned int flags) {194 __builtin_ia32_lwpval64(data2, data1, flags); // expected-error {{argument to '__builtin_ia32_lwpval64' must be a constant integer}}195}196