clang/test/CodeGen/X86/x86-intrinsics-imm.c

   1 // RUN: %clang_cc1 -triple x86_64-unknown-unknown -fsyntax-only \
   2 // RUN:  -target-feature +f16c -target-feature +avx -target-feature +sse4a \
   3 // RUN:  -target-feature +aes -target-feature +xop -target-feature +avx2 \
   4 // RUN:  -target-feature +tbm -verify %s
   5
   6 // Error test cases where a variable is passed to intrinsics but an
   7 // immediate operand is required.
   8
   9 // Don't include mm_malloc.h, it's system specific.
  10 #define __MM_MALLOC_H
  11
  12 #include <x86intrin.h>
  13
  14 unsigned short check__cvtss_sh(float val, const int I) {
  15   return _cvtss_sh(val, I); // expected-error {{argument to '__builtin_ia32_vcvtps2ph' must be a constant integer}}
  16 }
  17
  18 __m128i check__mm_cvtps_ph(__m128 val, const int I) {
  19   return _mm_cvtps_ph(val, I); // expected-error {{argument to '__builtin_ia32_vcvtps2ph' must be a constant integer}}
  20 }
  21
  22 __m128i check__mm256_cvtps_ph(__m256 val, const int I) {
  23   return _mm256_cvtps_ph(val, I); // expected-error  {{argument to '__builtin_ia32_vcvtps2ph256' must be a constant integer}}
  24 }
  25
  26 void check__mm_slli_si128(__m128i a, const int count) {
  27   _mm_slli_si128(a, count); // expected-error {{argument to '__builtin_ia32_pslldqi128_byteshift' must be a constant integer}}
  28 }
  29
  30 void check__mm_srli_si128(__m128i a, const int count) {
  31   _mm_srli_si128(a, count); // expected-error {{argument to '__builtin_ia32_psrldqi128_byteshift' must be a constant integer}}
  32 }
  33
  34 void check__mm_shuffle_epi32(__m128i  a, const int imm) {
  35   _mm_shuffle_epi32(a, imm); // expected-error {{argument to '__builtin_ia32_pshufd' must be a constant integer}}
  36 }
  37
  38 void check__mm_shufflelo_epi16(__m128i a, const int imm) {
  39   _mm_shufflelo_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshuflw' must be a constant integer}}
  40 }
  41
  42 void check__mm_shufflehi_epi16(__m128i a, const int imm) {
  43   _mm_shufflehi_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshufhw' must be a constant integer}}
  44 }
  45
  46 void check__mm_shuffle_pd(__m128d a, __m128d b, const int i) {
  47   _mm_shuffle_pd(a, b, i); // expected-error {{argument to '__builtin_ia32_shufpd' must be a constant integer}}
  48 }
  49
  50 void check__mm256_round_pd(__m256d a, const int b) {
  51   _mm256_round_pd(a, b); // expected-error {{argument to '__builtin_ia32_roundpd256' must be a constant integer}}
  52 }
  53
  54 void check__mm256_round_ps(__m256 a, const int b) {
  55   _mm256_round_ps(a, b); // expected-error {{argument to '__builtin_ia32_roundps256' must be a constant integer}}
  56 }
  57
  58 void check__mm_permute_pd(__m128d a, const int b) {
  59   _mm_permute_pd(a, b); // expected-error {{argument to '__builtin_ia32_vpermilpd' must be a constant integer}}
  60 }
  61
  62 void check__mm256_permute_pd(__m256d a, const int b) {
  63   _mm256_permute_pd(a, b); // expected-error {{argument to '__builtin_ia32_vpermilpd256' must be a constant integer}}
  64 }
  65
  66 void check__mm_permute_ps(__m128 a, const int b) {
  67   _mm_permute_ps(a, b); // expected-error {{argument to '__builtin_ia32_vpermilps' must be a constant integer}}
  68 }
  69
  70 void check__mm256_permute_ps(__m256 a, const int b) {
  71   _mm256_permute_ps(a, b); // expected-error {{argument to '__builtin_ia32_vpermilps256' must be a constant integer}}
  72 }
  73
  74 void check__mm256_permute2f128_pd(__m256d v1, __m256d v2, const char m) {
  75   _mm256_permute2f128_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_pd256' must be a constant integer}}
  76 }
  77
  78 void check__mm256_permute2f128_ps(__m256 v1, __m256 v2, const char m) {
  79   _mm256_permute2f128_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_ps256' must be a constant integer}}
  80 }
  81
  82 void check__mm256_permute2f128_si256(__m256i v1, __m256i v2, const char m) {
  83   _mm256_permute2f128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_vperm2f128_si256' must be a constant integer}}
  84 }
  85
  86 void check__m256_blend_pd(__m256d v1, __m256d v2, const char m) {
  87   _mm256_blend_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendpd256' must be a constant integer}}
  88 }
  89
  90 void check__m256_blend_ps(__m256 v1, __m256 v2, const char m) {
  91   _mm256_blend_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendps256' must be a constant integer}}
  92 }
  93
  94 void check__mm256_dp_ps(__m256 v1, __m256 v2, const char m) {
  95   _mm256_dp_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_dpps256' must be a constant integer}}
  96 }
  97
  98 void check__m256_shuffle_ps(__m256 a, __m256 b, const int m) {
  99   _mm256_shuffle_ps(a, b, m); // expected-error {{argument to '__builtin_ia32_shufps256' must be a constant integer}}
 100 }
 101
 102 void check__m256_shuffle_pd(__m256d a, __m256d b, const int m) {
 103   _mm256_shuffle_pd(a, b, m); // expected-error {{argument to '__builtin_ia32_shufpd256' must be a constant integer}}
 104 }
 105
 106 void check__mm_cmp_pd(__m128d a, __m128d b, const int c) {
 107   _mm_cmp_pd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmppd' must be a constant integer}}
 108 }
 109
 110 void check__mm_cmp_ps(__m128 a, __m128 b, const int c) {
 111   _mm_cmp_ps(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpps' must be a constant integer}}
 112 }
 113
 114 void check__mm256_cmp_pd(__m256d a, __m256d b, const int c) {
 115   _mm256_cmp_pd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmppd256' must be a constant integer}}
 116 }
 117
 118 void check__mm256_cmp_ps(__m256 a, __m256 b, const int c) {
 119   _mm256_cmp_ps(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpps256' must be a constant integer}}
 120 }
 121
 122 void check__mm_cmp_sd(__m128d a, __m128d b, const int c) {
 123   _mm_cmp_sd(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpsd' must be a constant integer}}
 124 }
 125
 126 void check__mm_cmp_ss(__m128 a, __m128 b, const int c) {
 127   _mm_cmp_ss(a, b, c); // expected-error {{argument to '__builtin_ia32_cmpss' must be a constant integer}}
 128 }
 129
 130 void check__mm256_extractf128_pd(__m256d a, const int o) {
 131   _mm256_extractf128_pd(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_pd256' must be a constant integer}}
 132 }
 133
 134 void check__mm256_extractf128_ps(__m256 a, const int o) {
 135   _mm256_extractf128_ps(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_ps256' must be a constant integer}}
 136 }
 137
 138 void check__mm256_extractf128_si256(__m256i a, const int o) {
 139   _mm256_extractf128_si256(a, o); // expected-error {{argument to '__builtin_ia32_vextractf128_si256' must be a constant integer}}
 140 }
 141
 142 void check__mm256_insertf128_pd(__m256d v1, __m128d v2, const int o) {
 143   _mm256_insertf128_pd(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_pd256' must be a constant integer}}
 144 }
 145
 146 void check__mm256_insertf128_ps(__m256 v1, __m128 v2, const int o) {
 147   _mm256_insertf128_ps(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_ps256' must be a constant integer}}
 148 }
 149
 150 void check__mm256_insertf128_si256(__m256i v1, __m128i v2, const int o) {
 151   _mm256_insertf128_si256(v1, v2, o); // expected-error {{argument to '__builtin_ia32_vinsertf128_si256' must be a constant integer}}
 152 }
 153
 154 void check__mm_round_ps(__m128 x, const int m) {
 155   _mm_round_ps(x, m); // expected-error {{argument to '__builtin_ia32_roundps' must be a constant integer}}
 156 }
 157
 158 void check__mm_round_ss(__m128 x, __m128 y, const int m) {
 159   _mm_round_ss(x, y, m); // expected-error {{argument to '__builtin_ia32_roundss' must be a constant integer}}
 160 }
 161
 162 void check__mm_round_pd(__m128d x, const int m) {
 163   _mm_round_pd(x, m); // expected-error {{argument to '__builtin_ia32_roundpd' must be a constant integer}}
 164 }
 165
 166 void check__mm_round_sd(__m128d x, __m128d y, const int m) {
 167   _mm_round_sd(x, y, m); // expected-error {{argument to '__builtin_ia32_roundsd' must be a constant integer}}
 168 }
 169
 170 void check__mm_blend_pd(__m128d v1, __m128d v2, const int m) {
 171   _mm_blend_pd(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendpd' must be a constant integer}}
 172 }
 173
 174 void check__mm_blend_ps(__m128 v1, __m128 v2, const int m) {
 175   _mm_blend_ps(v1, v2, m); // expected-error {{argument to '__builtin_ia32_blendps' must be a constant integer}}
 176 }
 177
 178 void check__mm_blend_epi16(__m128i v1, __m128i v2, const int m) {
 179   _mm_blend_epi16(v1, v2, m); // expected-error {{argument to '__builtin_ia32_pblendw128' must be a constant integer}}
 180 }
 181
 182 void check__mm_dp_ps(__m128 x, __m128 y, const int m) {
 183   _mm_dp_ps(x, y, m); // expected-error {{argument to '__builtin_ia32_dpps' must be a constant integer}}
 184 }
 185
 186 void check__mm_dp_pd(__m128d x, __m128d y, const int m) {
 187   _mm_dp_pd(x, y, m); // expected-error {{argument to '__builtin_ia32_dppd' must be a constant integer}}
 188 }
 189
 190 void check__mm_insert_ps(__m128 a, __m128 b, const int n) {
 191   _mm_insert_ps(a, b, n); // expected-error {{argument to '__builtin_ia32_insertps128' must be a constant integer}}
 192 }
 193
 194 void check__mm_mpsadbw_epu8(__m128i x, __m128i y, const int m) {
 195   _mm_mpsadbw_epu8(x, y, m); // expected-error {{argument to '__builtin_ia32_mpsadbw128' must be a constant integer}}
 196 }
 197
 198 void check__mm_cmpistrm(__m128 a, __m128 b, const int m) {
 199   _mm_cmpistrm(a, b, m); // expected-error {{argument to '__builtin_ia32_pcmpistrm128' must be a constant integer}}
 200 }
 201
 202 void check__mm_cmpistri(__m128i a, __m128i b, const int m) {
 203   _mm_cmpistri(a, b, m); // expected-error {{argument to '__builtin_ia32_pcmpistri128' must be a constant integer}}
 204 }
 205
 206 void check__mm_cmpestrm(__m128 a, int b, __m128 c, int d,  const int m) {
 207   _mm_cmpestrm(a, b, c, d, m); // expected-error {{argument to '__builtin_ia32_pcmpestrm128' must be a constant integer}}
 208 }
 209
 210 void check__mm_cmpestri(__m128i a, int b, __m128i c, int d,  const int m) {
 211   _mm_cmpestri(a, b, c, d, m); // expected-error {{argument to '__builtin_ia32_pcmpestri128' must be a constant integer}}
 212 }
 213
 214 void check__mm_alignr_epi8(__m128i a, __m128i b, const int n) {
 215   _mm_alignr_epi8(a, b, n); // expected-error {{argument to '__builtin_ia32_palignr128' must be a constant integer}}
 216 }
 217
 218 void check__mm_alignr_pi8(__m64 a, __m64 b, const int n) {
 219   _mm_alignr_pi8(a, b, n); // expected-error {{argument to '__builtin_ia32_psrldqi128_byteshift' must be a constant integer}}
 220 }
 221
 222 void check__mm_aeskeygenassist_si128(__m128 c, const int r) {
 223   _mm_aeskeygenassist_si128(c, r); // expected-error {{argument to '__builtin_ia32_aeskeygenassist128' must be a constant integer}}
 224 }
 225
 226 __m64 check__mm_shuffle_pi16(__m64 a, const int n) {
 227   return _mm_shuffle_pi16(a, n); // expected-error {{index for __builtin_shufflevector must be a constant integer}}
 228 }
 229
 230 void check__mm_shuffle_ps(__m128 a, __m128 b, const int m) {
 231   _mm_shuffle_ps(a, b, m); // expected-error {{argument to '__builtin_ia32_shufps' must be a constant integer}}
 232 }
 233
 234 void check__mm_com_epi8(__m128 a, __m128 b, const char c) {
 235   _mm_com_epi8(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomb' must be a constant integer}}
 236 }
 237
 238 void check__mm_com_epi16(__m128 a, __m128 b, const char c) {
 239   _mm_com_epi16(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomw' must be a constant integer}}
 240 }
 241
 242 void check__mm_com_epi32(__m128 a, __m128 b, const char c) {
 243   _mm_com_epi32(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomd' must be a constant integer}}
 244 }
 245
 246 void check__mm_com_epi64(__m128 a, __m128 b, const char c) {
 247   _mm_com_epi64(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomq' must be a constant integer}}
 248 }
 249
 250 void check__mm_com_epu8(__m128 a, __m128 b, const char c) {
 251   _mm_com_epu8(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomub' must be a constant integer}}
 252 }
 253
 254 void check__mm_com_epu16(__m128 a, __m128 b, const char c) {
 255   _mm_com_epu16(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomuw' must be a constant integer}}
 256 }
 257
 258 void check__mm_com_epu32(__m128 a, __m128 b, const char c) {
 259   _mm_com_epu32(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomud' must be a constant integer}}
 260 }
 261
 262 void check__mm_com_epu64(__m128 a, __m128 b, const char c) {
 263   _mm_com_epu64(a, b, c); // expected-error {{argument to '__builtin_ia32_vpcomuq' must be a constant integer}}
 264 }
 265
 266 void check__mm_permute2_pd(__m128d a, __m128d b, __m128d c, const char d) {
 267   _mm_permute2_pd(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2pd' must be a constant integer}}
 268 }
 269
 270 void check__mm_permute2_ps(__m128 a, __m128 b, __m128 c, const char d) {
 271   _mm_permute2_ps(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2ps' must be a constant integer}}
 272 }
 273
 274 void check__mm256_permute2_pd(__m256d a, __m256d b, __m256d c, const char d) {
 275   _mm256_permute2_pd(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2pd256' must be a constant integer}}
 276 }
 277
 278 void check__mm256_permute2_ps(__m256 a, __m256 b, __m256 c, const char d) {
 279   _mm256_permute2_ps(a, b, c, d); // expected-error {{argument to '__builtin_ia32_vpermil2ps256' must be a constant integer}}
 280 }
 281
 282 void check__mm_roti_epi8(__m128 a, const char b) {
 283   _mm_roti_epi8(a, b); // expected-error {{argument to '__builtin_ia32_vprotbi' must be a constant integer}}
 284 }
 285
 286 void check__mm_roti_epi16(__m128 a, const char b) {
 287   _mm_roti_epi16(a, b); // expected-error {{argument to '__builtin_ia32_vprotwi' must be a constant integer}}
 288 }
 289
 290 void check__mm_roti_epi32(__m128 a, const char b) {
 291   _mm_roti_epi32(a, b); // expected-error {{argument to '__builtin_ia32_vprotdi' must be a constant integer}}
 292 }
 293
 294 void check__mm_roti_epi64(__m128 a, const char b) {
 295   _mm_roti_epi64(a, b); // expected-error {{argument to '__builtin_ia32_vprotqi' must be a constant integer}}
 296 }
 297
 298 void check__mm256_mpsadbw_epu8(__m256i a, __m256i b, const int c) {
 299   _mm256_mpsadbw_epu8(a, b, c); // expected-error {{argument to '__builtin_ia32_mpsadbw256' must be a constant integer}}
 300 }
 301
 302 void check__mm256_alignr_epi8(__m256i a, __m256i b, const int n) {
 303   _mm256_alignr_epi8(a, b, n); // expected-error {{argument to '__builtin_ia32_palignr256' must be a constant integer}}
 304 }
 305
 306 void check__mm256_blend_epi16(__m256i a, __m256i b, const int m) {
 307   _mm256_blend_epi16(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendw256' must be a constant integer}}
 308 }
 309
 310 void check__mm256_slli_si256(__m256i a, const int count) {
 311   _mm256_slli_si256(a, count); // expected-error {{argument to '__builtin_ia32_pslldqi256_byteshift' must be a constant integer}}
 312 }
 313
 314 void check__mm256_shuffle_epi32(__m256i  a, const int imm) {
 315   _mm256_shuffle_epi32(a, imm); // expected-error {{argument to '__builtin_ia32_pshufd256' must be a constant integer}}
 316 }
 317
 318 void check__mm256_shufflehi_epi16(__m256i  a, const int imm) {
 319   _mm256_shufflehi_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshufhw256' must be a constant integer}}
 320 }
 321
 322 void check__mm256_shufflelo_epi16(__m256i  a, const int imm) {
 323   _mm256_shufflelo_epi16(a, imm); // expected-error {{argument to '__builtin_ia32_pshuflw256' must be a constant integer}}
 324 }
 325
 326 void check__mm_blend_epi32(__m128i a, __m128i b, const int m) {
 327   _mm_blend_epi32(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendd128' must be a constant integer}}
 328 }
 329
 330 void check__mm256_blend_epi32(__m256i a, __m256i b, const int m) {
 331   _mm256_blend_epi32(a, b, m); // expected-error {{argument to '__builtin_ia32_pblendd256' must be a constant integer}}
 332 }
 333
 334 void check__mm256_permute4x64_pd(__m256d v, const int m) {
 335   _mm256_permute4x64_pd(v, m); // expected-error {{argument to '__builtin_ia32_permdf256' must be a constant integer}}
 336 }
 337
 338 void check__mm256_permute4x64_epi64(__m256i v, const int m) {
 339   _mm256_permute4x64_epi64(v, m); // expected-error {{argument to '__builtin_ia32_permdi256' must be a constant integer}}
 340 }
 341
 342 void check__mm256_permute2x128_si256(__m256i v1, __m256i v2, const int m) {
 343   _mm256_permute2x128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_permti256' must be a constant integer}}
 344 }
 345
 346 void check__mm256_extracti128_si256(__m256i v1, const int m) {
 347   _mm256_extracti128_si256(v1, m); // expected-error {{argument to '__builtin_ia32_extract128i256' must be a constant integer}}
 348 }
 349
 350 void check__mm256_inserti128_si256(__m256i v1, __m128i v2, const int m) {
 351   _mm256_inserti128_si256(v1, v2, m); // expected-error {{argument to '__builtin_ia32_insert128i256' must be a constant integer}}
 352 }
 353
 354 void check__mm256_srli_si256(__m256i a, int count) {
 355   _mm256_srli_si256(a, count); // expected-error {{argument to '__builtin_ia32_psrldqi256_byteshift' must be a constant integer}}
 356 }
 357
 358 int check__bextri_u32(int a, int b) {
 359   return __bextri_u32(a, b); // expected-error {{argument to '__builtin_ia32_bextri_u32' must be a constant integer}}
 360 }
 361
 362 int check__bextri_u64(long a, long b) {
 363   return __bextri_u64(a, b); // expected-error {{argument to '__builtin_ia32_bextri_u64' must be a constant integer}}
 364 }
 365
 366 int check___builtin_eh_return_data_regno(int a) {
 367   return __builtin_eh_return_data_regno(a); // expected-error {{argument to '__builtin_eh_return_data_regno' must be a constant integer}}
 368 }
 369
 370 void* check___builtin_frame_address(unsigned int a) {
 371   return __builtin_frame_address(a); // expected-error {{argument to '__builtin_frame_address' must be a constant integer}}
 372 }
 373
 374 void* check___builtin_return_address(unsigned int a) {
 375   return __builtin_return_address(a); // expected-error {{argument to '__builtin_return_address' must be a constant integer}}
 376 }
 377
 378 void check__mm_extracti_si64(__m128i a, const char len, const char id) {
 379     _mm_extracti_si64(a, len, id); // expected-error {{argument to '__builtin_ia32_extrqi' must be a constant integer}}
 380 }
 381
 382 void check__insert_si64(__m128 a, __m128 b, const char len, const char id) {
 383     _mm_inserti_si64(a, b, len, id); // expected-error {{argument to '__builtin_ia32_insertqi' must be a constant integer}}
 384 }
 385