Skip to content

Commit 2e09664

Browse files
phoebewangtstellar
phoebewang
authored and
tstellar
committed
[X86] Backport saturate-convert intrinsics renaming & YMM rounding intrinsics removal in AVX10.2
AVX10.2 YMM rounding instructions are removed from latest AVX10 technical paper. Remove all intrinsics from compiler. AVX10.2 saturate-convert intrinsics are modified to use "s_" in the name. It is a consensus made with GCC folks to avoid future ambiguity.
1 parent 0dd4235 commit 2e09664

21 files changed

+1127
-6094
lines changed

‎clang/lib/Headers/avx10_2_512convertintrin.h‎

Lines changed: 24 additions & 22 deletions
Original file line numberDiff line numberDiff line change
@@ -78,20 +78,20 @@ _mm512_maskz_cvtbiasph_bf8(__mmask32 __U, __m512i __A, __m512h __B) {
7878
}
7979

8080
static __inline__ __m256i __DEFAULT_FN_ATTRS512
81-
_mm512_cvtbiassph_bf8(__m512i __A, __m512h __B) {
81+
_mm512_cvts_biasph_bf8(__m512i __A, __m512h __B) {
8282
return (__m256i)__builtin_ia32_vcvtbiasph2bf8s_512_mask(
8383
(__v64qi)__A, (__v32hf)__B, (__v32qi)_mm256_undefined_si256(),
8484
(__mmask32)-1);
8585
}
8686

87-
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_mask_cvtbiassph_bf8(
87+
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_mask_cvts_biasph_bf8(
8888
__m256i __W, __mmask32 __U, __m512i __A, __m512h __B) {
8989
return (__m256i)__builtin_ia32_vcvtbiasph2bf8s_512_mask(
9090
(__v64qi)__A, (__v32hf)__B, (__v32qi)(__m256i)__W, (__mmask32)__U);
9191
}
9292

9393
static __inline__ __m256i __DEFAULT_FN_ATTRS512
94-
_mm512_maskz_cvtbiassph_bf8(__mmask32 __U, __m512i __A, __m512h __B) {
94+
_mm512_maskz_cvts_biasph_bf8(__mmask32 __U, __m512i __A, __m512h __B) {
9595
return (__m256i)__builtin_ia32_vcvtbiasph2bf8s_512_mask(
9696
(__v64qi)__A, (__v32hf)__B, (__v32qi)(__m256i)_mm256_setzero_si256(),
9797
(__mmask32)__U);
@@ -118,20 +118,20 @@ _mm512_maskz_cvtbiasph_hf8(__mmask32 __U, __m512i __A, __m512h __B) {
118118
}
119119

120120
static __inline__ __m256i __DEFAULT_FN_ATTRS512
121-
_mm512_cvtbiassph_hf8(__m512i __A, __m512h __B) {
121+
_mm512_cvts_biasph_hf8(__m512i __A, __m512h __B) {
122122
return (__m256i)__builtin_ia32_vcvtbiasph2hf8s_512_mask(
123123
(__v64qi)__A, (__v32hf)__B, (__v32qi)_mm256_undefined_si256(),
124124
(__mmask32)-1);
125125
}
126126

127-
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_mask_cvtbiassph_hf8(
127+
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_mask_cvts_biasph_hf8(
128128
__m256i __W, __mmask32 __U, __m512i __A, __m512h __B) {
129129
return (__m256i)__builtin_ia32_vcvtbiasph2hf8s_512_mask(
130130
(__v64qi)__A, (__v32hf)__B, (__v32qi)(__m256i)__W, (__mmask32)__U);
131131
}
132132

133133
static __inline__ __m256i __DEFAULT_FN_ATTRS512
134-
_mm512_maskz_cvtbiassph_hf8(__mmask32 __U, __m512i __A, __m512h __B) {
134+
_mm512_maskz_cvts_biasph_hf8(__mmask32 __U, __m512i __A, __m512h __B) {
135135
return (__m256i)__builtin_ia32_vcvtbiasph2hf8s_512_mask(
136136
(__v64qi)__A, (__v32hf)__B, (__v32qi)(__m256i)_mm256_setzero_si256(),
137137
(__mmask32)__U);
@@ -157,21 +157,21 @@ _mm512_maskz_cvt2ph_bf8(__mmask64 __U, __m512h __A, __m512h __B) {
157157
}
158158

159159
static __inline__ __m512i __DEFAULT_FN_ATTRS512
160-
_mm512_cvts2ph_bf8(__m512h __A, __m512h __B) {
160+
_mm512_cvts_2ph_bf8(__m512h __A, __m512h __B) {
161161
return (__m512i)__builtin_ia32_vcvt2ph2bf8s_512((__v32hf)(__A),
162162
(__v32hf)(__B));
163163
}
164164

165165
static __inline__ __m512i __DEFAULT_FN_ATTRS512
166-
_mm512_mask_cvts2ph_bf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) {
166+
_mm512_mask_cvts_2ph_bf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) {
167167
return (__m512i)__builtin_ia32_selectb_512(
168-
(__mmask64)__U, (__v64qi)_mm512_cvts2ph_bf8(__A, __B), (__v64qi)__W);
168+
(__mmask64)__U, (__v64qi)_mm512_cvts_2ph_bf8(__A, __B), (__v64qi)__W);
169169
}
170170

171171
static __inline__ __m512i __DEFAULT_FN_ATTRS512
172-
_mm512_maskz_cvts2ph_bf8(__mmask64 __U, __m512h __A, __m512h __B) {
172+
_mm512_maskz_cvts_2ph_bf8(__mmask64 __U, __m512h __A, __m512h __B) {
173173
return (__m512i)__builtin_ia32_selectb_512(
174-
(__mmask64)__U, (__v64qi)_mm512_cvts2ph_bf8(__A, __B),
174+
(__mmask64)__U, (__v64qi)_mm512_cvts_2ph_bf8(__A, __B),
175175
(__v64qi)(__m512i)_mm512_setzero_si512());
176176
}
177177

@@ -195,21 +195,21 @@ _mm512_maskz_cvt2ph_hf8(__mmask64 __U, __m512h __A, __m512h __B) {
195195
}
196196

197197
static __inline__ __m512i __DEFAULT_FN_ATTRS512
198-
_mm512_cvts2ph_hf8(__m512h __A, __m512h __B) {
198+
_mm512_cvts_2ph_hf8(__m512h __A, __m512h __B) {
199199
return (__m512i)__builtin_ia32_vcvt2ph2hf8s_512((__v32hf)(__A),
200200
(__v32hf)(__B));
201201
}
202202

203203
static __inline__ __m512i __DEFAULT_FN_ATTRS512
204-
_mm512_mask_cvts2ph_hf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) {
204+
_mm512_mask_cvts_2ph_hf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) {
205205
return (__m512i)__builtin_ia32_selectb_512(
206-
(__mmask64)__U, (__v64qi)_mm512_cvts2ph_hf8(__A, __B), (__v64qi)__W);
206+
(__mmask64)__U, (__v64qi)_mm512_cvts_2ph_hf8(__A, __B), (__v64qi)__W);
207207
}
208208

209209
static __inline__ __m512i __DEFAULT_FN_ATTRS512
210-
_mm512_maskz_cvts2ph_hf8(__mmask64 __U, __m512h __A, __m512h __B) {
210+
_mm512_maskz_cvts_2ph_hf8(__mmask64 __U, __m512h __A, __m512h __B) {
211211
return (__m512i)__builtin_ia32_selectb_512(
212-
(__mmask64)__U, (__v64qi)_mm512_cvts2ph_hf8(__A, __B),
212+
(__mmask64)__U, (__v64qi)_mm512_cvts_2ph_hf8(__A, __B),
213213
(__v64qi)(__m512i)_mm512_setzero_si512());
214214
}
215215

@@ -247,19 +247,20 @@ _mm512_maskz_cvtph_bf8(__mmask32 __U, __m512h __A) {
247247
(__v32hf)__A, (__v32qi)(__m256i)_mm256_setzero_si256(), (__mmask32)__U);
248248
}
249249

250-
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_cvtsph_bf8(__m512h __A) {
250+
static __inline__ __m256i __DEFAULT_FN_ATTRS512
251+
_mm512_cvts_ph_bf8(__m512h __A) {
251252
return (__m256i)__builtin_ia32_vcvtph2bf8s_512_mask(
252253
(__v32hf)__A, (__v32qi)(__m256i)_mm256_undefined_si256(), (__mmask32)-1);
253254
}
254255

255256
static __inline__ __m256i __DEFAULT_FN_ATTRS512
256-
_mm512_mask_cvtsph_bf8(__m256i __W, __mmask32 __U, __m512h __A) {
257+
_mm512_mask_cvts_ph_bf8(__m256i __W, __mmask32 __U, __m512h __A) {
257258
return (__m256i)__builtin_ia32_vcvtph2bf8s_512_mask(
258259
(__v32hf)__A, (__v32qi)(__m256i)__W, (__mmask32)__U);
259260
}
260261

261262
static __inline__ __m256i __DEFAULT_FN_ATTRS512
262-
_mm512_maskz_cvtsph_bf8(__mmask32 __U, __m512h __A) {
263+
_mm512_maskz_cvts_ph_bf8(__mmask32 __U, __m512h __A) {
263264
return (__m256i)__builtin_ia32_vcvtph2bf8s_512_mask(
264265
(__v32hf)__A, (__v32qi)(__m256i)_mm256_setzero_si256(), (__mmask32)__U);
265266
}
@@ -281,19 +282,20 @@ _mm512_maskz_cvtph_hf8(__mmask32 __U, __m512h __A) {
281282
(__v32hf)__A, (__v32qi)(__m256i)_mm256_setzero_si256(), (__mmask32)__U);
282283
}
283284

284-
static __inline__ __m256i __DEFAULT_FN_ATTRS512 _mm512_cvtsph_hf8(__m512h __A) {
285+
static __inline__ __m256i __DEFAULT_FN_ATTRS512
286+
_mm512_cvts_ph_hf8(__m512h __A) {
285287
return (__m256i)__builtin_ia32_vcvtph2hf8s_512_mask(
286288
(__v32hf)__A, (__v32qi)(__m256i)_mm256_undefined_si256(), (__mmask32)-1);
287289
}
288290

289291
static __inline__ __m256i __DEFAULT_FN_ATTRS512
290-
_mm512_mask_cvtsph_hf8(__m256i __W, __mmask32 __U, __m512h __A) {
292+
_mm512_mask_cvts_ph_hf8(__m256i __W, __mmask32 __U, __m512h __A) {
291293
return (__m256i)__builtin_ia32_vcvtph2hf8s_512_mask(
292294
(__v32hf)__A, (__v32qi)(__m256i)__W, (__mmask32)__U);
293295
}
294296

295297
static __inline__ __m256i __DEFAULT_FN_ATTRS512
296-
_mm512_maskz_cvtsph_hf8(__mmask32 __U, __m512h __A) {
298+
_mm512_maskz_cvts_ph_hf8(__mmask32 __U, __m512h __A) {
297299
return (__m256i)__builtin_ia32_vcvtph2hf8s_512_mask(
298300
(__v32hf)__A, (__v32qi)(__m256i)_mm256_setzero_si256(), (__mmask32)__U);
299301
}

‎clang/lib/Headers/avx10_2_512satcvtdsintrin.h‎

Lines changed: 28 additions & 24 deletions
Original file line numberDiff line numberDiff line change
@@ -20,20 +20,21 @@
2020
__min_vector_width__(512)))
2121

2222
// 512 bit : Double -> Int
23-
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm512_cvttspd_epi32(__m512d __A) {
23+
static __inline__ __m256i __DEFAULT_FN_ATTRS
24+
_mm512_cvtts_pd_epi32(__m512d __A) {
2425
return ((__m256i)__builtin_ia32_vcvttpd2dqs512_round_mask(
2526
(__v8df)__A, (__v8si)_mm256_undefined_si256(), (__mmask8)-1,
2627
_MM_FROUND_CUR_DIRECTION));
2728
}
2829

2930
static __inline__ __m256i __DEFAULT_FN_ATTRS
30-
_mm512_mask_cvttspd_epi32(__m256i __W, __mmask8 __U, __m512d __A) {
31+
_mm512_mask_cvtts_pd_epi32(__m256i __W, __mmask8 __U, __m512d __A) {
3132
return ((__m256i)__builtin_ia32_vcvttpd2dqs512_round_mask(
3233
(__v8df)__A, (__v8si)__W, __U, _MM_FROUND_CUR_DIRECTION));
3334
}
3435

3536
static __inline__ __m256i __DEFAULT_FN_ATTRS
36-
_mm512_maskz_cvttspd_epi32(__mmask8 __U, __m512d __A) {
37+
_mm512_maskz_cvtts_pd_epi32(__mmask8 __U, __m512d __A) {
3738
return ((__m256i)__builtin_ia32_vcvttpd2dqs512_round_mask(
3839
(__v8df)__A, (__v8si)_mm256_setzero_si256(), __U,
3940
_MM_FROUND_CUR_DIRECTION));
@@ -55,20 +56,21 @@ _mm512_maskz_cvttspd_epi32(__mmask8 __U, __m512d __A) {
5556
(const int)(__R)))
5657

5758
// 512 bit : Double -> uInt
58-
static __inline__ __m256i __DEFAULT_FN_ATTRS _mm512_cvttspd_epu32(__m512d __A) {
59+
static __inline__ __m256i __DEFAULT_FN_ATTRS
60+
_mm512_cvtts_pd_epu32(__m512d __A) {
5961
return ((__m256i)__builtin_ia32_vcvttpd2udqs512_round_mask(
6062
(__v8df)__A, (__v8si)_mm256_undefined_si256(), (__mmask8)-1,
6163
_MM_FROUND_CUR_DIRECTION));
6264
}
6365

6466
static __inline__ __m256i __DEFAULT_FN_ATTRS
65-
_mm512_mask_cvttspd_epu32(__m256i __W, __mmask8 __U, __m512d __A) {
67+
_mm512_mask_cvtts_pd_epu32(__m256i __W, __mmask8 __U, __m512d __A) {
6668
return ((__m256i)__builtin_ia32_vcvttpd2udqs512_round_mask(
6769
(__v8df)__A, (__v8si)__W, __U, _MM_FROUND_CUR_DIRECTION));
6870
}
6971

7072
static __inline__ __m256i __DEFAULT_FN_ATTRS
71-
_mm512_maskz_cvttspd_epu32(__mmask8 __U, __m512d __A) {
73+
_mm512_maskz_cvtts_pd_epu32(__mmask8 __U, __m512d __A) {
7274
return ((__m256i)__builtin_ia32_vcvttpd2udqs512_round_mask(
7375
(__v8df)__A, (__v8si)_mm256_setzero_si256(), __U,
7476
_MM_FROUND_CUR_DIRECTION));
@@ -91,18 +93,19 @@ _mm512_maskz_cvttspd_epu32(__mmask8 __U, __m512d __A) {
9193

9294
// 512 bit : Double -> Long
9395

94-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttspd_epi64(__m512d __A) {
96+
static __inline__ __m512i __DEFAULT_FN_ATTRS
97+
_mm512_cvtts_pd_epi64(__m512d __A) {
9598
return ((__m512i)__builtin_ia32_vcvttpd2qqs512_round_mask(
9699
(__v8df)__A, (__v8di)_mm512_undefined_epi32(), (__mmask8)-1,
97100
_MM_FROUND_CUR_DIRECTION));
98101
}
99102
static __inline__ __m512i __DEFAULT_FN_ATTRS
100-
_mm512_mask_cvttspd_epi64(__m512i __W, __mmask8 __U, __m512d __A) {
103+
_mm512_mask_cvtts_pd_epi64(__m512i __W, __mmask8 __U, __m512d __A) {
101104
return ((__m512i)__builtin_ia32_vcvttpd2qqs512_round_mask(
102105
(__v8df)__A, (__v8di)__W, __U, _MM_FROUND_CUR_DIRECTION));
103106
}
104107
static __inline__ __m512i __DEFAULT_FN_ATTRS
105-
_mm512_maskz_cvttspd_epi64(__mmask8 __U, __m512d __A) {
108+
_mm512_maskz_cvtts_pd_epi64(__mmask8 __U, __m512d __A) {
106109
return ((__m512i)__builtin_ia32_vcvttpd2qqs512_round_mask(
107110
(__v8df)__A, (__v8di)_mm512_setzero_si512(), __U,
108111
_MM_FROUND_CUR_DIRECTION));
@@ -125,20 +128,21 @@ _mm512_maskz_cvttspd_epi64(__mmask8 __U, __m512d __A) {
125128

126129
// 512 bit : Double -> ULong
127130

128-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttspd_epu64(__m512d __A) {
131+
static __inline__ __m512i __DEFAULT_FN_ATTRS
132+
_mm512_cvtts_pd_epu64(__m512d __A) {
129133
return ((__m512i)__builtin_ia32_vcvttpd2uqqs512_round_mask(
130134
(__v8df)__A, (__v8di)_mm512_undefined_epi32(), (__mmask8)-1,
131135
_MM_FROUND_CUR_DIRECTION));
132136
}
133137

134138
static __inline__ __m512i __DEFAULT_FN_ATTRS
135-
_mm512_mask_cvttspd_epu64(__m512i __W, __mmask8 __U, __m512d __A) {
139+
_mm512_mask_cvtts_pd_epu64(__m512i __W, __mmask8 __U, __m512d __A) {
136140
return ((__m512i)__builtin_ia32_vcvttpd2uqqs512_round_mask(
137141
(__v8df)__A, (__v8di)__W, __U, _MM_FROUND_CUR_DIRECTION));
138142
}
139143

140144
static __inline__ __m512i __DEFAULT_FN_ATTRS
141-
_mm512_maskz_cvttspd_epu64(__mmask8 __U, __m512d __A) {
145+
_mm512_maskz_cvtts_pd_epu64(__mmask8 __U, __m512d __A) {
142146
return ((__m512i)__builtin_ia32_vcvttpd2uqqs512_round_mask(
143147
(__v8df)__A, (__v8di)_mm512_setzero_si512(), __U,
144148
_MM_FROUND_CUR_DIRECTION));
@@ -160,20 +164,20 @@ _mm512_maskz_cvttspd_epu64(__mmask8 __U, __m512d __A) {
160164
(const int)(__R)))
161165

162166
// 512 bit: Float -> int
163-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttsps_epi32(__m512 __A) {
167+
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvtts_ps_epi32(__m512 __A) {
164168
return ((__m512i)__builtin_ia32_vcvttps2dqs512_round_mask(
165169
(__v16sf)(__A), (__v16si)_mm512_undefined_epi32(), (__mmask16)-1,
166170
_MM_FROUND_CUR_DIRECTION));
167171
}
168172

169173
static __inline__ __m512i __DEFAULT_FN_ATTRS
170-
_mm512_mask_cvttsps_epi32(__m512i __W, __mmask16 __U, __m512 __A) {
174+
_mm512_mask_cvtts_ps_epi32(__m512i __W, __mmask16 __U, __m512 __A) {
171175
return ((__m512i)__builtin_ia32_vcvttps2dqs512_round_mask(
172176
(__v16sf)(__A), (__v16si)(__W), __U, _MM_FROUND_CUR_DIRECTION));
173177
}
174178

175179
static __inline__ __m512i __DEFAULT_FN_ATTRS
176-
_mm512_maskz_cvttsps_epi32(__mmask16 __U, __m512 __A) {
180+
_mm512_maskz_cvtts_ps_epi32(__mmask16 __U, __m512 __A) {
177181
return ((__m512i)__builtin_ia32_vcvttps2dqs512_round_mask(
178182
(__v16sf)(__A), (__v16si)_mm512_setzero_si512(), __U,
179183
_MM_FROUND_CUR_DIRECTION));
@@ -195,20 +199,20 @@ _mm512_maskz_cvttsps_epi32(__mmask16 __U, __m512 __A) {
195199
(__mmask16)(__U), (const int)(__R)))
196200

197201
// 512 bit: Float -> uint
198-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttsps_epu32(__m512 __A) {
202+
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvtts_ps_epu32(__m512 __A) {
199203
return ((__m512i)__builtin_ia32_vcvttps2udqs512_round_mask(
200204
(__v16sf)(__A), (__v16si)_mm512_undefined_epi32(), (__mmask16)-1,
201205
_MM_FROUND_CUR_DIRECTION));
202206
}
203207

204208
static __inline__ __m512i __DEFAULT_FN_ATTRS
205-
_mm512_mask_cvttsps_epu32(__m512i __W, __mmask16 __U, __m512 __A) {
209+
_mm512_mask_cvtts_ps_epu32(__m512i __W, __mmask16 __U, __m512 __A) {
206210
return ((__m512i)__builtin_ia32_vcvttps2udqs512_round_mask(
207211
(__v16sf)(__A), (__v16si)(__W), __U, _MM_FROUND_CUR_DIRECTION));
208212
}
209213

210214
static __inline__ __m512i __DEFAULT_FN_ATTRS
211-
_mm512_maskz_cvttsps_epu32(__mmask16 __U, __m512 __A) {
215+
_mm512_maskz_cvtts_ps_epu32(__mmask16 __U, __m512 __A) {
212216
return ((__m512i)__builtin_ia32_vcvttps2udqs512_round_mask(
213217
(__v16sf)(__A), (__v16si)_mm512_setzero_si512(), __U,
214218
_MM_FROUND_CUR_DIRECTION));
@@ -230,20 +234,20 @@ _mm512_maskz_cvttsps_epu32(__mmask16 __U, __m512 __A) {
230234
(__mmask16)(__U), (const int)(__R)))
231235

232236
// 512 bit : float -> long
233-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttsps_epi64(__m256 __A) {
237+
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvtts_ps_epi64(__m256 __A) {
234238
return ((__m512i)__builtin_ia32_vcvttps2qqs512_round_mask(
235239
(__v8sf)__A, (__v8di)_mm512_undefined_epi32(), (__mmask8)-1,
236240
_MM_FROUND_CUR_DIRECTION));
237241
}
238242

239243
static __inline__ __m512i __DEFAULT_FN_ATTRS
240-
_mm512_mask_cvttsps_epi64(__m512i __W, __mmask8 __U, __m256 __A) {
244+
_mm512_mask_cvtts_ps_epi64(__m512i __W, __mmask8 __U, __m256 __A) {
241245
return ((__m512i)__builtin_ia32_vcvttps2qqs512_round_mask(
242246
(__v8sf)__A, (__v8di)__W, __U, _MM_FROUND_CUR_DIRECTION));
243247
}
244248

245249
static __inline__ __m512i __DEFAULT_FN_ATTRS
246-
_mm512_maskz_cvttsps_epi64(__mmask8 __U, __m256 __A) {
250+
_mm512_maskz_cvtts_ps_epi64(__mmask8 __U, __m256 __A) {
247251
return ((__m512i)__builtin_ia32_vcvttps2qqs512_round_mask(
248252
(__v8sf)__A, (__v8di)_mm512_setzero_si512(), __U,
249253
_MM_FROUND_CUR_DIRECTION));
@@ -265,20 +269,20 @@ _mm512_maskz_cvttsps_epi64(__mmask8 __U, __m256 __A) {
265269
(const int)(__R)))
266270

267271
// 512 bit : float -> ulong
268-
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvttsps_epu64(__m256 __A) {
272+
static __inline__ __m512i __DEFAULT_FN_ATTRS _mm512_cvtts_ps_epu64(__m256 __A) {
269273
return ((__m512i)__builtin_ia32_vcvttps2uqqs512_round_mask(
270274
(__v8sf)__A, (__v8di)_mm512_undefined_epi32(), (__mmask8)-1,
271275
_MM_FROUND_CUR_DIRECTION));
272276
}
273277

274278
static __inline__ __m512i __DEFAULT_FN_ATTRS
275-
_mm512_mask_cvttsps_epu64(__m512i __W, __mmask8 __U, __m256 __A) {
279+
_mm512_mask_cvtts_ps_epu64(__m512i __W, __mmask8 __U, __m256 __A) {
276280
return ((__m512i)__builtin_ia32_vcvttps2uqqs512_round_mask(
277281
(__v8sf)__A, (__v8di)__W, __U, _MM_FROUND_CUR_DIRECTION));
278282
}
279283

280284
static __inline__ __m512i __DEFAULT_FN_ATTRS
281-
_mm512_maskz_cvttsps_epu64(__mmask8 __U, __m256 __A) {
285+
_mm512_maskz_cvtts_ps_epu64(__mmask8 __U, __m256 __A) {
282286
return ((__m512i)__builtin_ia32_vcvttps2uqqs512_round_mask(
283287
(__v8sf)__A, (__v8di)_mm512_setzero_si512(), __U,
284288
_MM_FROUND_CUR_DIRECTION));

0 commit comments

Comments
 (0)