Skip to content

Commit 7fe0691

Browse files
ahmednoursphinxahmednoursphinx
authored
[Headers][X86] Allow AVX512 masked shuffles to be used in constexpr (#162301)
This PR makes AVX512 masked shuffle and broadcast intrinsics usable in constexpr Fixes #162074
1 parent 733fe42 commit 7fe0691

File tree

8 files changed

+329
-357
lines changed

8 files changed

+329
-357
lines changed

‎clang/lib/Headers/avx512dqintrin.h‎

Lines changed: 24 additions & 36 deletions
Original file line numberDiff line numberDiff line change
@@ -1083,17 +1083,15 @@ _mm512_broadcast_f32x2(__m128 __A) {
10831083
0, 1, 0, 1, 0, 1, 0, 1);
10841084
}
10851085

1086-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
1087-
_mm512_mask_broadcast_f32x2 (__m512 __O, __mmask16 __M, __m128 __A)
1088-
{
1086+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
1087+
_mm512_mask_broadcast_f32x2(__m512 __O, __mmask16 __M, __m128 __A) {
10891088
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
10901089
(__v16sf)_mm512_broadcast_f32x2(__A),
10911090
(__v16sf)__O);
10921091
}
10931092

1094-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
1095-
_mm512_maskz_broadcast_f32x2 (__mmask16 __M, __m128 __A)
1096-
{
1093+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
1094+
_mm512_maskz_broadcast_f32x2(__mmask16 __M, __m128 __A) {
10971095
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
10981096
(__v16sf)_mm512_broadcast_f32x2(__A),
10991097
(__v16sf)_mm512_setzero_ps());
@@ -1106,17 +1104,15 @@ _mm512_broadcast_f32x8(__m256 __A) {
11061104
0, 1, 2, 3, 4, 5, 6, 7);
11071105
}
11081106

1109-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
1110-
_mm512_mask_broadcast_f32x8(__m512 __O, __mmask16 __M, __m256 __A)
1111-
{
1107+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
1108+
_mm512_mask_broadcast_f32x8(__m512 __O, __mmask16 __M, __m256 __A) {
11121109
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
11131110
(__v16sf)_mm512_broadcast_f32x8(__A),
11141111
(__v16sf)__O);
11151112
}
11161113

1117-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
1118-
_mm512_maskz_broadcast_f32x8(__mmask16 __M, __m256 __A)
1119-
{
1114+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
1115+
_mm512_maskz_broadcast_f32x8(__mmask16 __M, __m256 __A) {
11201116
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
11211117
(__v16sf)_mm512_broadcast_f32x8(__A),
11221118
(__v16sf)_mm512_setzero_ps());
@@ -1128,17 +1124,15 @@ _mm512_broadcast_f64x2(__m128d __A) {
11281124
0, 1, 0, 1, 0, 1, 0, 1);
11291125
}
11301126

1131-
static __inline__ __m512d __DEFAULT_FN_ATTRS512
1132-
_mm512_mask_broadcast_f64x2(__m512d __O, __mmask8 __M, __m128d __A)
1133-
{
1127+
static __inline__ __m512d __DEFAULT_FN_ATTRS512_CONSTEXPR
1128+
_mm512_mask_broadcast_f64x2(__m512d __O, __mmask8 __M, __m128d __A) {
11341129
return (__m512d)__builtin_ia32_selectpd_512((__mmask8)__M,
11351130
(__v8df)_mm512_broadcast_f64x2(__A),
11361131
(__v8df)__O);
11371132
}
11381133

1139-
static __inline__ __m512d __DEFAULT_FN_ATTRS512
1140-
_mm512_maskz_broadcast_f64x2(__mmask8 __M, __m128d __A)
1141-
{
1134+
static __inline__ __m512d __DEFAULT_FN_ATTRS512_CONSTEXPR
1135+
_mm512_maskz_broadcast_f64x2(__mmask8 __M, __m128d __A) {
11421136
return (__m512d)__builtin_ia32_selectpd_512((__mmask8)__M,
11431137
(__v8df)_mm512_broadcast_f64x2(__A),
11441138
(__v8df)_mm512_setzero_pd());
@@ -1151,17 +1145,15 @@ _mm512_broadcast_i32x2(__m128i __A) {
11511145
0, 1, 0, 1, 0, 1, 0, 1);
11521146
}
11531147

1154-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1155-
_mm512_mask_broadcast_i32x2 (__m512i __O, __mmask16 __M, __m128i __A)
1156-
{
1148+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1149+
_mm512_mask_broadcast_i32x2(__m512i __O, __mmask16 __M, __m128i __A) {
11571150
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
11581151
(__v16si)_mm512_broadcast_i32x2(__A),
11591152
(__v16si)__O);
11601153
}
11611154

1162-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1163-
_mm512_maskz_broadcast_i32x2 (__mmask16 __M, __m128i __A)
1164-
{
1155+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1156+
_mm512_maskz_broadcast_i32x2(__mmask16 __M, __m128i __A) {
11651157
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
11661158
(__v16si)_mm512_broadcast_i32x2(__A),
11671159
(__v16si)_mm512_setzero_si512());
@@ -1174,17 +1166,15 @@ _mm512_broadcast_i32x8(__m256i __A) {
11741166
0, 1, 2, 3, 4, 5, 6, 7);
11751167
}
11761168

1177-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1178-
_mm512_mask_broadcast_i32x8(__m512i __O, __mmask16 __M, __m256i __A)
1179-
{
1169+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1170+
_mm512_mask_broadcast_i32x8(__m512i __O, __mmask16 __M, __m256i __A) {
11801171
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
11811172
(__v16si)_mm512_broadcast_i32x8(__A),
11821173
(__v16si)__O);
11831174
}
11841175

1185-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1186-
_mm512_maskz_broadcast_i32x8(__mmask16 __M, __m256i __A)
1187-
{
1176+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1177+
_mm512_maskz_broadcast_i32x8(__mmask16 __M, __m256i __A) {
11881178
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
11891179
(__v16si)_mm512_broadcast_i32x8(__A),
11901180
(__v16si)_mm512_setzero_si512());
@@ -1196,17 +1186,15 @@ _mm512_broadcast_i64x2(__m128i __A) {
11961186
0, 1, 0, 1, 0, 1, 0, 1);
11971187
}
11981188

1199-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1200-
_mm512_mask_broadcast_i64x2(__m512i __O, __mmask8 __M, __m128i __A)
1201-
{
1189+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1190+
_mm512_mask_broadcast_i64x2(__m512i __O, __mmask8 __M, __m128i __A) {
12021191
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__M,
12031192
(__v8di)_mm512_broadcast_i64x2(__A),
12041193
(__v8di)__O);
12051194
}
12061195

1207-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
1208-
_mm512_maskz_broadcast_i64x2(__mmask8 __M, __m128i __A)
1209-
{
1196+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
1197+
_mm512_maskz_broadcast_i64x2(__mmask8 __M, __m128i __A) {
12101198
return (__m512i)__builtin_ia32_selectq_512((__mmask8)__M,
12111199
(__v8di)_mm512_broadcast_i64x2(__A),
12121200
(__v8di)_mm512_setzero_si512());

‎clang/lib/Headers/avx512fintrin.h‎

Lines changed: 50 additions & 76 deletions
Original file line numberDiff line numberDiff line change
@@ -225,17 +225,15 @@ _mm512_broadcastd_epi32(__m128i __A) {
225225
0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0, 0);
226226
}
227227

228-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
229-
_mm512_mask_broadcastd_epi32 (__m512i __O, __mmask16 __M, __m128i __A)
230-
{
228+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
229+
_mm512_mask_broadcastd_epi32(__m512i __O, __mmask16 __M, __m128i __A) {
231230
return (__m512i)__builtin_ia32_selectd_512(__M,
232231
(__v16si) _mm512_broadcastd_epi32(__A),
233232
(__v16si) __O);
234233
}
235234

236-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
237-
_mm512_maskz_broadcastd_epi32 (__mmask16 __M, __m128i __A)
238-
{
235+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
236+
_mm512_maskz_broadcastd_epi32(__mmask16 __M, __m128i __A) {
239237
return (__m512i)__builtin_ia32_selectd_512(__M,
240238
(__v16si) _mm512_broadcastd_epi32(__A),
241239
(__v16si) _mm512_setzero_si512());
@@ -247,18 +245,14 @@ _mm512_broadcastq_epi64(__m128i __A) {
247245
0, 0, 0, 0, 0, 0, 0, 0);
248246
}
249247

250-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
251-
_mm512_mask_broadcastq_epi64 (__m512i __O, __mmask8 __M, __m128i __A)
252-
{
253-
return (__m512i)__builtin_ia32_selectq_512(__M,
254-
(__v8di) _mm512_broadcastq_epi64(__A),
255-
(__v8di) __O);
256-
248+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
249+
_mm512_mask_broadcastq_epi64(__m512i __O, __mmask8 __M, __m128i __A) {
250+
return (__m512i)__builtin_ia32_selectq_512(
251+
__M, (__v8di)_mm512_broadcastq_epi64(__A), (__v8di)__O);
257252
}
258253

259-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
260-
_mm512_maskz_broadcastq_epi64 (__mmask8 __M, __m128i __A)
261-
{
254+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
255+
_mm512_maskz_broadcastq_epi64(__mmask8 __M, __m128i __A) {
262256
return (__m512i)__builtin_ia32_selectq_512(__M,
263257
(__v8di) _mm512_broadcastq_epi64(__A),
264258
(__v8di) _mm512_setzero_si512());
@@ -321,9 +315,8 @@ _mm512_set1_epi32(int __s)
321315
__s, __s, __s, __s, __s, __s, __s, __s };
322316
}
323317

324-
static __inline __m512i __DEFAULT_FN_ATTRS512
325-
_mm512_maskz_set1_epi32(__mmask16 __M, int __A)
326-
{
318+
static __inline __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
319+
_mm512_maskz_set1_epi32(__mmask16 __M, int __A) {
327320
return (__m512i)__builtin_ia32_selectd_512(__M,
328321
(__v16si)_mm512_set1_epi32(__A),
329322
(__v16si)_mm512_setzero_si512());
@@ -335,9 +328,8 @@ _mm512_set1_epi64(long long __d)
335328
return __extension__(__m512i)(__v8di){ __d, __d, __d, __d, __d, __d, __d, __d };
336329
}
337330

338-
static __inline __m512i __DEFAULT_FN_ATTRS512
339-
_mm512_maskz_set1_epi64(__mmask8 __M, long long __A)
340-
{
331+
static __inline __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
332+
_mm512_maskz_set1_epi64(__mmask8 __M, long long __A) {
341333
return (__m512i)__builtin_ia32_selectq_512(__M,
342334
(__v8di)_mm512_set1_epi64(__A),
343335
(__v8di)_mm512_setzero_si512());
@@ -6552,17 +6544,15 @@ _mm512_broadcast_f32x4(__m128 __A) {
65526544
0, 1, 2, 3, 0, 1, 2, 3);
65536545
}
65546546

6555-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
6556-
_mm512_mask_broadcast_f32x4(__m512 __O, __mmask16 __M, __m128 __A)
6557-
{
6547+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
6548+
_mm512_mask_broadcast_f32x4(__m512 __O, __mmask16 __M, __m128 __A) {
65586549
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
65596550
(__v16sf)_mm512_broadcast_f32x4(__A),
65606551
(__v16sf)__O);
65616552
}
65626553

6563-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
6564-
_mm512_maskz_broadcast_f32x4(__mmask16 __M, __m128 __A)
6565-
{
6554+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
6555+
_mm512_maskz_broadcast_f32x4(__mmask16 __M, __m128 __A) {
65666556
return (__m512)__builtin_ia32_selectps_512((__mmask16)__M,
65676557
(__v16sf)_mm512_broadcast_f32x4(__A),
65686558
(__v16sf)_mm512_setzero_ps());
@@ -6597,17 +6587,15 @@ _mm512_broadcast_i32x4(__m128i __A) {
65976587
0, 1, 2, 3, 0, 1, 2, 3);
65986588
}
65996589

6600-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
6601-
_mm512_mask_broadcast_i32x4(__m512i __O, __mmask16 __M, __m128i __A)
6602-
{
6590+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
6591+
_mm512_mask_broadcast_i32x4(__m512i __O, __mmask16 __M, __m128i __A) {
66036592
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
66046593
(__v16si)_mm512_broadcast_i32x4(__A),
66056594
(__v16si)__O);
66066595
}
66076596

6608-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
6609-
_mm512_maskz_broadcast_i32x4(__mmask16 __M, __m128i __A)
6610-
{
6597+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
6598+
_mm512_maskz_broadcast_i32x4(__mmask16 __M, __m128i __A) {
66116599
return (__m512i)__builtin_ia32_selectd_512((__mmask16)__M,
66126600
(__v16si)_mm512_broadcast_i32x4(__A),
66136601
(__v16si)_mm512_setzero_si512());
@@ -6635,33 +6623,29 @@ _mm512_maskz_broadcast_i64x4(__mmask8 __M, __m256i __A)
66356623
(__v8di)_mm512_setzero_si512());
66366624
}
66376625

6638-
static __inline__ __m512d __DEFAULT_FN_ATTRS512
6639-
_mm512_mask_broadcastsd_pd (__m512d __O, __mmask8 __M, __m128d __A)
6640-
{
6626+
static __inline__ __m512d __DEFAULT_FN_ATTRS512_CONSTEXPR
6627+
_mm512_mask_broadcastsd_pd(__m512d __O, __mmask8 __M, __m128d __A) {
66416628
return (__m512d)__builtin_ia32_selectpd_512(__M,
66426629
(__v8df) _mm512_broadcastsd_pd(__A),
66436630
(__v8df) __O);
66446631
}
66456632

6646-
static __inline__ __m512d __DEFAULT_FN_ATTRS512
6647-
_mm512_maskz_broadcastsd_pd (__mmask8 __M, __m128d __A)
6648-
{
6633+
static __inline__ __m512d __DEFAULT_FN_ATTRS512_CONSTEXPR
6634+
_mm512_maskz_broadcastsd_pd(__mmask8 __M, __m128d __A) {
66496635
return (__m512d)__builtin_ia32_selectpd_512(__M,
66506636
(__v8df) _mm512_broadcastsd_pd(__A),
66516637
(__v8df) _mm512_setzero_pd());
66526638
}
66536639

6654-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
6655-
_mm512_mask_broadcastss_ps (__m512 __O, __mmask16 __M, __m128 __A)
6656-
{
6640+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
6641+
_mm512_mask_broadcastss_ps(__m512 __O, __mmask16 __M, __m128 __A) {
66576642
return (__m512)__builtin_ia32_selectps_512(__M,
66586643
(__v16sf) _mm512_broadcastss_ps(__A),
66596644
(__v16sf) __O);
66606645
}
66616646

6662-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
6663-
_mm512_maskz_broadcastss_ps (__mmask16 __M, __m128 __A)
6664-
{
6647+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
6648+
_mm512_maskz_broadcastss_ps(__mmask16 __M, __m128 __A) {
66656649
return (__m512)__builtin_ia32_selectps_512(__M,
66666650
(__v16sf) _mm512_broadcastss_ps(__A),
66676651
(__v16sf) _mm512_setzero_ps());
@@ -8381,17 +8365,15 @@ _mm512_movehdup_ps (__m512 __A)
83818365
1, 1, 3, 3, 5, 5, 7, 7, 9, 9, 11, 11, 13, 13, 15, 15);
83828366
}
83838367

8384-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
8385-
_mm512_mask_movehdup_ps (__m512 __W, __mmask16 __U, __m512 __A)
8386-
{
8368+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
8369+
_mm512_mask_movehdup_ps(__m512 __W, __mmask16 __U, __m512 __A) {
83878370
return (__m512)__builtin_ia32_selectps_512((__mmask16)__U,
83888371
(__v16sf)_mm512_movehdup_ps(__A),
83898372
(__v16sf)__W);
83908373
}
83918374

8392-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
8393-
_mm512_maskz_movehdup_ps (__mmask16 __U, __m512 __A)
8394-
{
8375+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
8376+
_mm512_maskz_movehdup_ps(__mmask16 __U, __m512 __A) {
83958377
return (__m512)__builtin_ia32_selectps_512((__mmask16)__U,
83968378
(__v16sf)_mm512_movehdup_ps(__A),
83978379
(__v16sf)_mm512_setzero_ps());
@@ -8404,44 +8386,38 @@ _mm512_moveldup_ps (__m512 __A)
84048386
0, 0, 2, 2, 4, 4, 6, 6, 8, 8, 10, 10, 12, 12, 14, 14);
84058387
}
84068388

8407-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
8408-
_mm512_mask_moveldup_ps (__m512 __W, __mmask16 __U, __m512 __A)
8409-
{
8389+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
8390+
_mm512_mask_moveldup_ps(__m512 __W, __mmask16 __U, __m512 __A) {
84108391
return (__m512)__builtin_ia32_selectps_512((__mmask16)__U,
84118392
(__v16sf)_mm512_moveldup_ps(__A),
84128393
(__v16sf)__W);
84138394
}
84148395

8415-
static __inline__ __m512 __DEFAULT_FN_ATTRS512
8416-
_mm512_maskz_moveldup_ps (__mmask16 __U, __m512 __A)
8417-
{
8396+
static __inline__ __m512 __DEFAULT_FN_ATTRS512_CONSTEXPR
8397+
_mm512_maskz_moveldup_ps(__mmask16 __U, __m512 __A) {
84188398
return (__m512)__builtin_ia32_selectps_512((__mmask16)__U,
84198399
(__v16sf)_mm512_moveldup_ps(__A),
84208400
(__v16sf)_mm512_setzero_ps());
84218401
}
84228402

8423-
static __inline__ __m128 __DEFAULT_FN_ATTRS128
8424-
_mm_mask_move_ss (__m128 __W, __mmask8 __U, __m128 __A, __m128 __B)
8425-
{
8403+
static __inline__ __m128 __DEFAULT_FN_ATTRS128_CONSTEXPR
8404+
_mm_mask_move_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B) {
84268405
return __builtin_ia32_selectss_128(__U, _mm_move_ss(__A, __B), __W);
84278406
}
84288407

8429-
static __inline__ __m128 __DEFAULT_FN_ATTRS128
8430-
_mm_maskz_move_ss (__mmask8 __U, __m128 __A, __m128 __B)
8431-
{
8408+
static __inline__ __m128 __DEFAULT_FN_ATTRS128_CONSTEXPR
8409+
_mm_maskz_move_ss(__mmask8 __U, __m128 __A, __m128 __B) {
84328410
return __builtin_ia32_selectss_128(__U, _mm_move_ss(__A, __B),
84338411
_mm_setzero_ps());
84348412
}
84358413

8436-
static __inline__ __m128d __DEFAULT_FN_ATTRS128
8437-
_mm_mask_move_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B)
8438-
{
8414+
static __inline__ __m128d __DEFAULT_FN_ATTRS128_CONSTEXPR
8415+
_mm_mask_move_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B) {
84398416
return __builtin_ia32_selectsd_128(__U, _mm_move_sd(__A, __B), __W);
84408417
}
84418418

8442-
static __inline__ __m128d __DEFAULT_FN_ATTRS128
8443-
_mm_maskz_move_sd (__mmask8 __U, __m128d __A, __m128d __B)
8444-
{
8419+
static __inline__ __m128d __DEFAULT_FN_ATTRS128_CONSTEXPR
8420+
_mm_maskz_move_sd(__mmask8 __U, __m128d __A, __m128d __B) {
84458421
return __builtin_ia32_selectsd_128(__U, _mm_move_sd(__A, __B),
84468422
_mm_setzero_pd());
84478423
}
@@ -8884,17 +8860,15 @@ _mm_cvtu64_ss (__m128 __A, unsigned long long __B)
88848860
}
88858861
#endif
88868862

8887-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
8888-
_mm512_mask_set1_epi32 (__m512i __O, __mmask16 __M, int __A)
8889-
{
8863+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
8864+
_mm512_mask_set1_epi32(__m512i __O, __mmask16 __M, int __A) {
88908865
return (__m512i) __builtin_ia32_selectd_512(__M,
88918866
(__v16si) _mm512_set1_epi32(__A),
88928867
(__v16si) __O);
88938868
}
88948869

8895-
static __inline__ __m512i __DEFAULT_FN_ATTRS512
8896-
_mm512_mask_set1_epi64 (__m512i __O, __mmask8 __M, long long __A)
8897-
{
8870+
static __inline__ __m512i __DEFAULT_FN_ATTRS512_CONSTEXPR
8871+
_mm512_mask_set1_epi64(__m512i __O, __mmask8 __M, long long __A) {
88988872
return (__m512i) __builtin_ia32_selectq_512(__M,
88998873
(__v8di) _mm512_set1_epi64(__A),
89008874
(__v8di) __O);

0 commit comments

Comments
 (0)