1 /* Copyright (C) 2014-2018 Free Software Foundation, Inc.
3 This file is part of GCC.
5 GCC is free software; you can redistribute it and/or modify
6 it under the terms of the GNU General Public License as published by
7 the Free Software Foundation; either version 3, or (at your option)
10 GCC is distributed in the hope that it will be useful,
11 but WITHOUT ANY WARRANTY; without even the implied warranty of
12 MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
13 GNU General Public License for more details.
15 Under Section 7 of GPL version 3, you are granted additional
16 permissions described in the GCC Runtime Library Exception, version
17 3.1, as published by the Free Software Foundation.
19 You should have received a copy of the GNU General Public License and
20 a copy of the GCC Runtime Library Exception along with this program;
21 see the files COPYING3 and COPYING.RUNTIME respectively. If not, see
22 <http://www.gnu.org/licenses/>. */
24 #ifndef _IMMINTRIN_H_INCLUDED
25 #error "Never use <avx512dqintrin.h> directly; include <immintrin.h> instead."
28 #ifndef _AVX512DQINTRIN_H_INCLUDED
29 #define _AVX512DQINTRIN_H_INCLUDED
32 #pragma GCC push_options
33 #pragma GCC target("avx512dq")
34 #define __DISABLE_AVX512DQ__
35 #endif /* __AVX512DQ__ */
37 extern __inline unsigned char
38 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
39 _ktest_mask8_u8 (__mmask8 __A, __mmask8 __B, unsigned char *__CF)
41 *__CF = (unsigned char) __builtin_ia32_ktestcqi (__A, __B);
42 return (unsigned char) __builtin_ia32_ktestzqi (__A, __B);
45 extern __inline unsigned char
46 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
47 _ktestz_mask8_u8 (__mmask8 __A, __mmask8 __B)
49 return (unsigned char) __builtin_ia32_ktestzqi (__A, __B);
52 extern __inline unsigned char
53 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
54 _ktestc_mask8_u8 (__mmask8 __A, __mmask8 __B)
56 return (unsigned char) __builtin_ia32_ktestcqi (__A, __B);
59 extern __inline unsigned char
60 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
61 _ktest_mask16_u8 (__mmask16 __A, __mmask16 __B, unsigned char *__CF)
63 *__CF = (unsigned char) __builtin_ia32_ktestchi (__A, __B);
64 return (unsigned char) __builtin_ia32_ktestzhi (__A, __B);
67 extern __inline unsigned char
68 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
69 _ktestz_mask16_u8 (__mmask16 __A, __mmask16 __B)
71 return (unsigned char) __builtin_ia32_ktestzhi (__A, __B);
74 extern __inline unsigned char
75 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
76 _ktestc_mask16_u8 (__mmask16 __A, __mmask16 __B)
78 return (unsigned char) __builtin_ia32_ktestchi (__A, __B);
81 extern __inline unsigned char
82 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
83 _kortest_mask8_u8 (__mmask8 __A, __mmask8 __B, unsigned char *__CF)
85 *__CF = (unsigned char) __builtin_ia32_kortestcqi (__A, __B);
86 return (unsigned char) __builtin_ia32_kortestzqi (__A, __B);
89 extern __inline unsigned char
90 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
91 _kortestz_mask8_u8 (__mmask8 __A, __mmask8 __B)
93 return (unsigned char) __builtin_ia32_kortestzqi (__A, __B);
96 extern __inline unsigned char
97 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
98 _kortestc_mask8_u8 (__mmask8 __A, __mmask8 __B)
100 return (unsigned char) __builtin_ia32_kortestcqi (__A, __B);
103 extern __inline __mmask8
104 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
105 _kadd_mask8 (__mmask8 __A, __mmask8 __B)
107 return (__mmask8) __builtin_ia32_kaddqi ((__mmask8) __A, (__mmask8) __B);
110 extern __inline __mmask16
111 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
112 _kadd_mask16 (__mmask16 __A, __mmask16 __B)
114 return (__mmask16) __builtin_ia32_kaddhi ((__mmask16) __A, (__mmask16) __B);
117 extern __inline unsigned int
118 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
119 _cvtmask8_u32 (__mmask8 __A)
121 return (unsigned int) __builtin_ia32_kmovb ((__mmask8 ) __A);
124 extern __inline __mmask8
125 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
126 _cvtu32_mask8 (unsigned int __A)
128 return (__mmask8) __builtin_ia32_kmovb ((__mmask8) __A);
131 extern __inline __mmask8
132 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
133 _load_mask8 (__mmask8 *__A)
135 return (__mmask8) __builtin_ia32_kmovb (*(__mmask8 *) __A);
139 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
140 _store_mask8 (__mmask8 *__A, __mmask8 __B)
142 *(__mmask8 *) __A = __builtin_ia32_kmovb (__B);
145 extern __inline __mmask8
146 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
147 _knot_mask8 (__mmask8 __A)
149 return (__mmask8) __builtin_ia32_knotqi ((__mmask8) __A);
152 extern __inline __mmask8
153 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
154 _kor_mask8 (__mmask8 __A, __mmask8 __B)
156 return (__mmask8) __builtin_ia32_korqi ((__mmask8) __A, (__mmask8) __B);
159 extern __inline __mmask8
160 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
161 _kxnor_mask8 (__mmask8 __A, __mmask8 __B)
163 return (__mmask8) __builtin_ia32_kxnorqi ((__mmask8) __A, (__mmask8) __B);
166 extern __inline __mmask8
167 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
168 _kxor_mask8 (__mmask8 __A, __mmask8 __B)
170 return (__mmask8) __builtin_ia32_kxorqi ((__mmask8) __A, (__mmask8) __B);
173 extern __inline __mmask8
174 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
175 _kand_mask8 (__mmask8 __A, __mmask8 __B)
177 return (__mmask8) __builtin_ia32_kandqi ((__mmask8) __A, (__mmask8) __B);
180 extern __inline __mmask8
181 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
182 _kandn_mask8 (__mmask8 __A, __mmask8 __B)
184 return (__mmask8) __builtin_ia32_kandnqi ((__mmask8) __A, (__mmask8) __B);
187 extern __inline __m512d
188 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
189 _mm512_broadcast_f64x2 (__m128d __A)
192 __builtin_ia32_broadcastf64x2_512_mask ((__v2df) __A,
193 _mm512_undefined_pd (),
197 extern __inline __m512d
198 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
199 _mm512_mask_broadcast_f64x2 (__m512d __O, __mmask8 __M, __m128d __A)
201 return (__m512d) __builtin_ia32_broadcastf64x2_512_mask ((__v2df)
207 extern __inline __m512d
208 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
209 _mm512_maskz_broadcast_f64x2 (__mmask8 __M, __m128d __A)
211 return (__m512d) __builtin_ia32_broadcastf64x2_512_mask ((__v2df)
214 _mm512_setzero_ps (),
218 extern __inline __m512i
219 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
220 _mm512_broadcast_i64x2 (__m128i __A)
223 __builtin_ia32_broadcasti64x2_512_mask ((__v2di) __A,
224 _mm512_undefined_epi32 (),
228 extern __inline __m512i
229 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
230 _mm512_mask_broadcast_i64x2 (__m512i __O, __mmask8 __M, __m128i __A)
232 return (__m512i) __builtin_ia32_broadcasti64x2_512_mask ((__v2di)
238 extern __inline __m512i
239 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
240 _mm512_maskz_broadcast_i64x2 (__mmask8 __M, __m128i __A)
242 return (__m512i) __builtin_ia32_broadcasti64x2_512_mask ((__v2di)
245 _mm512_setzero_si512 (),
249 extern __inline __m512
250 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
251 _mm512_broadcast_f32x2 (__m128 __A)
254 __builtin_ia32_broadcastf32x2_512_mask ((__v4sf) __A,
255 (__v16sf)_mm512_undefined_ps (),
259 extern __inline __m512
260 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
261 _mm512_mask_broadcast_f32x2 (__m512 __O, __mmask16 __M, __m128 __A)
263 return (__m512) __builtin_ia32_broadcastf32x2_512_mask ((__v4sf) __A,
268 extern __inline __m512
269 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
270 _mm512_maskz_broadcast_f32x2 (__mmask16 __M, __m128 __A)
272 return (__m512) __builtin_ia32_broadcastf32x2_512_mask ((__v4sf) __A,
274 _mm512_setzero_ps (),
278 extern __inline __m512i
279 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
280 _mm512_broadcast_i32x2 (__m128i __A)
283 __builtin_ia32_broadcasti32x2_512_mask ((__v4si) __A,
285 _mm512_undefined_epi32 (),
289 extern __inline __m512i
290 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
291 _mm512_mask_broadcast_i32x2 (__m512i __O, __mmask16 __M, __m128i __A)
293 return (__m512i) __builtin_ia32_broadcasti32x2_512_mask ((__v4si)
299 extern __inline __m512i
300 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
301 _mm512_maskz_broadcast_i32x2 (__mmask16 __M, __m128i __A)
303 return (__m512i) __builtin_ia32_broadcasti32x2_512_mask ((__v4si)
306 _mm512_setzero_si512 (),
310 extern __inline __m512
311 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
312 _mm512_broadcast_f32x8 (__m256 __A)
315 __builtin_ia32_broadcastf32x8_512_mask ((__v8sf) __A,
316 _mm512_undefined_ps (),
320 extern __inline __m512
321 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
322 _mm512_mask_broadcast_f32x8 (__m512 __O, __mmask16 __M, __m256 __A)
324 return (__m512) __builtin_ia32_broadcastf32x8_512_mask ((__v8sf) __A,
329 extern __inline __m512
330 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
331 _mm512_maskz_broadcast_f32x8 (__mmask16 __M, __m256 __A)
333 return (__m512) __builtin_ia32_broadcastf32x8_512_mask ((__v8sf) __A,
335 _mm512_setzero_ps (),
339 extern __inline __m512i
340 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
341 _mm512_broadcast_i32x8 (__m256i __A)
344 __builtin_ia32_broadcasti32x8_512_mask ((__v8si) __A,
346 _mm512_undefined_epi32 (),
350 extern __inline __m512i
351 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
352 _mm512_mask_broadcast_i32x8 (__m512i __O, __mmask16 __M, __m256i __A)
354 return (__m512i) __builtin_ia32_broadcasti32x8_512_mask ((__v8si)
360 extern __inline __m512i
361 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
362 _mm512_maskz_broadcast_i32x8 (__mmask16 __M, __m256i __A)
364 return (__m512i) __builtin_ia32_broadcasti32x8_512_mask ((__v8si)
367 _mm512_setzero_si512 (),
371 extern __inline __m512i
372 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
373 _mm512_mullo_epi64 (__m512i __A, __m512i __B)
375 return (__m512i) ((__v8du) __A * (__v8du) __B);
378 extern __inline __m512i
379 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
380 _mm512_mask_mullo_epi64 (__m512i __W, __mmask8 __U, __m512i __A,
383 return (__m512i) __builtin_ia32_pmullq512_mask ((__v8di) __A,
389 extern __inline __m512i
390 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
391 _mm512_maskz_mullo_epi64 (__mmask8 __U, __m512i __A, __m512i __B)
393 return (__m512i) __builtin_ia32_pmullq512_mask ((__v8di) __A,
396 _mm512_setzero_si512 (),
400 extern __inline __m512d
401 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
402 _mm512_xor_pd (__m512d __A, __m512d __B)
404 return (__m512d) __builtin_ia32_xorpd512_mask ((__v8df) __A,
407 _mm512_setzero_pd (),
411 extern __inline __m512d
412 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
413 _mm512_mask_xor_pd (__m512d __W, __mmask8 __U, __m512d __A,
416 return (__m512d) __builtin_ia32_xorpd512_mask ((__v8df) __A,
422 extern __inline __m512d
423 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
424 _mm512_maskz_xor_pd (__mmask8 __U, __m512d __A, __m512d __B)
426 return (__m512d) __builtin_ia32_xorpd512_mask ((__v8df) __A,
429 _mm512_setzero_pd (),
433 extern __inline __m512
434 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
435 _mm512_xor_ps (__m512 __A, __m512 __B)
437 return (__m512) __builtin_ia32_xorps512_mask ((__v16sf) __A,
440 _mm512_setzero_ps (),
444 extern __inline __m512
445 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
446 _mm512_mask_xor_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B)
448 return (__m512) __builtin_ia32_xorps512_mask ((__v16sf) __A,
454 extern __inline __m512
455 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
456 _mm512_maskz_xor_ps (__mmask16 __U, __m512 __A, __m512 __B)
458 return (__m512) __builtin_ia32_xorps512_mask ((__v16sf) __A,
461 _mm512_setzero_ps (),
465 extern __inline __m512d
466 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
467 _mm512_or_pd (__m512d __A, __m512d __B)
469 return (__m512d) __builtin_ia32_orpd512_mask ((__v8df) __A,
472 _mm512_setzero_pd (),
476 extern __inline __m512d
477 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
478 _mm512_mask_or_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B)
480 return (__m512d) __builtin_ia32_orpd512_mask ((__v8df) __A,
486 extern __inline __m512d
487 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
488 _mm512_maskz_or_pd (__mmask8 __U, __m512d __A, __m512d __B)
490 return (__m512d) __builtin_ia32_orpd512_mask ((__v8df) __A,
493 _mm512_setzero_pd (),
497 extern __inline __m512
498 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
499 _mm512_or_ps (__m512 __A, __m512 __B)
501 return (__m512) __builtin_ia32_orps512_mask ((__v16sf) __A,
504 _mm512_setzero_ps (),
508 extern __inline __m512
509 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
510 _mm512_mask_or_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B)
512 return (__m512) __builtin_ia32_orps512_mask ((__v16sf) __A,
518 extern __inline __m512
519 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
520 _mm512_maskz_or_ps (__mmask16 __U, __m512 __A, __m512 __B)
522 return (__m512) __builtin_ia32_orps512_mask ((__v16sf) __A,
525 _mm512_setzero_ps (),
529 extern __inline __m512d
530 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
531 _mm512_and_pd (__m512d __A, __m512d __B)
533 return (__m512d) __builtin_ia32_andpd512_mask ((__v8df) __A,
536 _mm512_setzero_pd (),
540 extern __inline __m512d
541 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
542 _mm512_mask_and_pd (__m512d __W, __mmask8 __U, __m512d __A,
545 return (__m512d) __builtin_ia32_andpd512_mask ((__v8df) __A,
551 extern __inline __m512d
552 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
553 _mm512_maskz_and_pd (__mmask8 __U, __m512d __A, __m512d __B)
555 return (__m512d) __builtin_ia32_andpd512_mask ((__v8df) __A,
558 _mm512_setzero_pd (),
562 extern __inline __m512
563 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
564 _mm512_and_ps (__m512 __A, __m512 __B)
566 return (__m512) __builtin_ia32_andps512_mask ((__v16sf) __A,
569 _mm512_setzero_ps (),
573 extern __inline __m512
574 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
575 _mm512_mask_and_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B)
577 return (__m512) __builtin_ia32_andps512_mask ((__v16sf) __A,
583 extern __inline __m512
584 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
585 _mm512_maskz_and_ps (__mmask16 __U, __m512 __A, __m512 __B)
587 return (__m512) __builtin_ia32_andps512_mask ((__v16sf) __A,
590 _mm512_setzero_ps (),
594 extern __inline __m512d
595 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
596 _mm512_andnot_pd (__m512d __A, __m512d __B)
598 return (__m512d) __builtin_ia32_andnpd512_mask ((__v8df) __A,
601 _mm512_setzero_pd (),
605 extern __inline __m512d
606 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
607 _mm512_mask_andnot_pd (__m512d __W, __mmask8 __U, __m512d __A,
610 return (__m512d) __builtin_ia32_andnpd512_mask ((__v8df) __A,
616 extern __inline __m512d
617 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
618 _mm512_maskz_andnot_pd (__mmask8 __U, __m512d __A, __m512d __B)
620 return (__m512d) __builtin_ia32_andnpd512_mask ((__v8df) __A,
623 _mm512_setzero_pd (),
627 extern __inline __m512
628 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
629 _mm512_andnot_ps (__m512 __A, __m512 __B)
631 return (__m512) __builtin_ia32_andnps512_mask ((__v16sf) __A,
634 _mm512_setzero_ps (),
638 extern __inline __m512
639 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
640 _mm512_mask_andnot_ps (__m512 __W, __mmask16 __U, __m512 __A,
643 return (__m512) __builtin_ia32_andnps512_mask ((__v16sf) __A,
649 extern __inline __m512
650 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
651 _mm512_maskz_andnot_ps (__mmask16 __U, __m512 __A, __m512 __B)
653 return (__m512) __builtin_ia32_andnps512_mask ((__v16sf) __A,
656 _mm512_setzero_ps (),
660 extern __inline __mmask16
661 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
662 _mm512_movepi32_mask (__m512i __A)
664 return (__mmask16) __builtin_ia32_cvtd2mask512 ((__v16si) __A);
667 extern __inline __mmask8
668 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
669 _mm512_movepi64_mask (__m512i __A)
671 return (__mmask8) __builtin_ia32_cvtq2mask512 ((__v8di) __A);
674 extern __inline __m512i
675 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
676 _mm512_movm_epi32 (__mmask16 __A)
678 return (__m512i) __builtin_ia32_cvtmask2d512 (__A);
681 extern __inline __m512i
682 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
683 _mm512_movm_epi64 (__mmask8 __A)
685 return (__m512i) __builtin_ia32_cvtmask2q512 (__A);
688 extern __inline __m512i
689 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
690 _mm512_cvttpd_epi64 (__m512d __A)
692 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
694 _mm512_setzero_si512 (),
696 _MM_FROUND_CUR_DIRECTION);
699 extern __inline __m512i
700 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
701 _mm512_mask_cvttpd_epi64 (__m512i __W, __mmask8 __U, __m512d __A)
703 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
706 _MM_FROUND_CUR_DIRECTION);
709 extern __inline __m512i
710 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
711 _mm512_maskz_cvttpd_epi64 (__mmask8 __U, __m512d __A)
713 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
715 _mm512_setzero_si512 (),
717 _MM_FROUND_CUR_DIRECTION);
720 extern __inline __m512i
721 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
722 _mm512_cvttpd_epu64 (__m512d __A)
724 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
726 _mm512_setzero_si512 (),
728 _MM_FROUND_CUR_DIRECTION);
731 extern __inline __m512i
732 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
733 _mm512_mask_cvttpd_epu64 (__m512i __W, __mmask8 __U, __m512d __A)
735 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
738 _MM_FROUND_CUR_DIRECTION);
741 extern __inline __m512i
742 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
743 _mm512_maskz_cvttpd_epu64 (__mmask8 __U, __m512d __A)
745 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
747 _mm512_setzero_si512 (),
749 _MM_FROUND_CUR_DIRECTION);
752 extern __inline __m512i
753 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
754 _mm512_cvttps_epi64 (__m256 __A)
756 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
758 _mm512_setzero_si512 (),
760 _MM_FROUND_CUR_DIRECTION);
763 extern __inline __m512i
764 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
765 _mm512_mask_cvttps_epi64 (__m512i __W, __mmask8 __U, __m256 __A)
767 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
770 _MM_FROUND_CUR_DIRECTION);
773 extern __inline __m512i
774 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
775 _mm512_maskz_cvttps_epi64 (__mmask8 __U, __m256 __A)
777 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
779 _mm512_setzero_si512 (),
781 _MM_FROUND_CUR_DIRECTION);
784 extern __inline __m512i
785 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
786 _mm512_cvttps_epu64 (__m256 __A)
788 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
790 _mm512_setzero_si512 (),
792 _MM_FROUND_CUR_DIRECTION);
795 extern __inline __m512i
796 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
797 _mm512_mask_cvttps_epu64 (__m512i __W, __mmask8 __U, __m256 __A)
799 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
802 _MM_FROUND_CUR_DIRECTION);
805 extern __inline __m512i
806 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
807 _mm512_maskz_cvttps_epu64 (__mmask8 __U, __m256 __A)
809 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
811 _mm512_setzero_si512 (),
813 _MM_FROUND_CUR_DIRECTION);
816 extern __inline __m512i
817 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
818 _mm512_cvtpd_epi64 (__m512d __A)
820 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
822 _mm512_setzero_si512 (),
824 _MM_FROUND_CUR_DIRECTION);
827 extern __inline __m512i
828 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
829 _mm512_mask_cvtpd_epi64 (__m512i __W, __mmask8 __U, __m512d __A)
831 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
834 _MM_FROUND_CUR_DIRECTION);
837 extern __inline __m512i
838 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
839 _mm512_maskz_cvtpd_epi64 (__mmask8 __U, __m512d __A)
841 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
843 _mm512_setzero_si512 (),
845 _MM_FROUND_CUR_DIRECTION);
848 extern __inline __m512i
849 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
850 _mm512_cvtpd_epu64 (__m512d __A)
852 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
854 _mm512_setzero_si512 (),
856 _MM_FROUND_CUR_DIRECTION);
859 extern __inline __m512i
860 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
861 _mm512_mask_cvtpd_epu64 (__m512i __W, __mmask8 __U, __m512d __A)
863 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
866 _MM_FROUND_CUR_DIRECTION);
869 extern __inline __m512i
870 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
871 _mm512_maskz_cvtpd_epu64 (__mmask8 __U, __m512d __A)
873 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
875 _mm512_setzero_si512 (),
877 _MM_FROUND_CUR_DIRECTION);
880 extern __inline __m512i
881 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
882 _mm512_cvtps_epi64 (__m256 __A)
884 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
886 _mm512_setzero_si512 (),
888 _MM_FROUND_CUR_DIRECTION);
891 extern __inline __m512i
892 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
893 _mm512_mask_cvtps_epi64 (__m512i __W, __mmask8 __U, __m256 __A)
895 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
898 _MM_FROUND_CUR_DIRECTION);
901 extern __inline __m512i
902 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
903 _mm512_maskz_cvtps_epi64 (__mmask8 __U, __m256 __A)
905 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
907 _mm512_setzero_si512 (),
909 _MM_FROUND_CUR_DIRECTION);
912 extern __inline __m512i
913 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
914 _mm512_cvtps_epu64 (__m256 __A)
916 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
918 _mm512_setzero_si512 (),
920 _MM_FROUND_CUR_DIRECTION);
923 extern __inline __m512i
924 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
925 _mm512_mask_cvtps_epu64 (__m512i __W, __mmask8 __U, __m256 __A)
927 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
930 _MM_FROUND_CUR_DIRECTION);
933 extern __inline __m512i
934 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
935 _mm512_maskz_cvtps_epu64 (__mmask8 __U, __m256 __A)
937 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
939 _mm512_setzero_si512 (),
941 _MM_FROUND_CUR_DIRECTION);
944 extern __inline __m256
945 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
946 _mm512_cvtepi64_ps (__m512i __A)
948 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
950 _mm256_setzero_ps (),
952 _MM_FROUND_CUR_DIRECTION);
955 extern __inline __m256
956 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
957 _mm512_mask_cvtepi64_ps (__m256 __W, __mmask8 __U, __m512i __A)
959 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
962 _MM_FROUND_CUR_DIRECTION);
965 extern __inline __m256
966 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
967 _mm512_maskz_cvtepi64_ps (__mmask8 __U, __m512i __A)
969 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
971 _mm256_setzero_ps (),
973 _MM_FROUND_CUR_DIRECTION);
976 extern __inline __m256
977 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
978 _mm512_cvtepu64_ps (__m512i __A)
980 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
982 _mm256_setzero_ps (),
984 _MM_FROUND_CUR_DIRECTION);
987 extern __inline __m256
988 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
989 _mm512_mask_cvtepu64_ps (__m256 __W, __mmask8 __U, __m512i __A)
991 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
994 _MM_FROUND_CUR_DIRECTION);
997 extern __inline __m256
998 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
999 _mm512_maskz_cvtepu64_ps (__mmask8 __U, __m512i __A)
1001 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
1003 _mm256_setzero_ps (),
1005 _MM_FROUND_CUR_DIRECTION);
1008 extern __inline __m512d
1009 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1010 _mm512_cvtepi64_pd (__m512i __A)
1012 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1014 _mm512_setzero_pd (),
1016 _MM_FROUND_CUR_DIRECTION);
1019 extern __inline __m512d
1020 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1021 _mm512_mask_cvtepi64_pd (__m512d __W, __mmask8 __U, __m512i __A)
1023 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1026 _MM_FROUND_CUR_DIRECTION);
1029 extern __inline __m512d
1030 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1031 _mm512_maskz_cvtepi64_pd (__mmask8 __U, __m512i __A)
1033 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1035 _mm512_setzero_pd (),
1037 _MM_FROUND_CUR_DIRECTION);
1040 extern __inline __m512d
1041 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1042 _mm512_cvtepu64_pd (__m512i __A)
1044 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1046 _mm512_setzero_pd (),
1048 _MM_FROUND_CUR_DIRECTION);
1051 extern __inline __m512d
1052 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1053 _mm512_mask_cvtepu64_pd (__m512d __W, __mmask8 __U, __m512i __A)
1055 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1058 _MM_FROUND_CUR_DIRECTION);
1061 extern __inline __m512d
1062 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1063 _mm512_maskz_cvtepu64_pd (__mmask8 __U, __m512i __A)
1065 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1067 _mm512_setzero_pd (),
1069 _MM_FROUND_CUR_DIRECTION);
1073 extern __inline __mmask8
1074 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1075 _kshiftli_mask8 (__mmask8 __A, unsigned int __B)
1077 return (__mmask8) __builtin_ia32_kshiftliqi ((__mmask8) __A, (__mmask8) __B);
1080 extern __inline __mmask8
1081 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1082 _kshiftri_mask8 (__mmask8 __A, unsigned int __B)
1084 return (__mmask8) __builtin_ia32_kshiftriqi ((__mmask8) __A, (__mmask8) __B);
1087 extern __inline __m512d
1088 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1089 _mm512_range_pd (__m512d __A, __m512d __B, int __C)
1091 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
1094 _mm512_setzero_pd (),
1096 _MM_FROUND_CUR_DIRECTION);
1099 extern __inline __m512d
1100 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1101 _mm512_mask_range_pd (__m512d __W, __mmask8 __U,
1102 __m512d __A, __m512d __B, int __C)
1104 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
1108 _MM_FROUND_CUR_DIRECTION);
1111 extern __inline __m512d
1112 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1113 _mm512_maskz_range_pd (__mmask8 __U, __m512d __A, __m512d __B, int __C)
1115 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
1118 _mm512_setzero_pd (),
1120 _MM_FROUND_CUR_DIRECTION);
1123 extern __inline __m512
1124 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1125 _mm512_range_ps (__m512 __A, __m512 __B, int __C)
1127 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
1130 _mm512_setzero_ps (),
1132 _MM_FROUND_CUR_DIRECTION);
1135 extern __inline __m512
1136 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1137 _mm512_mask_range_ps (__m512 __W, __mmask16 __U,
1138 __m512 __A, __m512 __B, int __C)
1140 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
1144 _MM_FROUND_CUR_DIRECTION);
1147 extern __inline __m512
1148 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1149 _mm512_maskz_range_ps (__mmask16 __U, __m512 __A, __m512 __B, int __C)
1151 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
1154 _mm512_setzero_ps (),
1156 _MM_FROUND_CUR_DIRECTION);
1159 extern __inline __m128d
1160 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1161 _mm_reduce_sd (__m128d __A, __m128d __B, int __C)
1163 return (__m128d) __builtin_ia32_reducesd_mask ((__v2df) __A,
1165 (__v2df) _mm_setzero_pd (),
1169 extern __inline __m128d
1170 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1171 _mm_mask_reduce_sd (__m128d __W, __mmask8 __U, __m128d __A,
1172 __m128d __B, int __C)
1174 return (__m128d) __builtin_ia32_reducesd_mask ((__v2df) __A,
1180 extern __inline __m128d
1181 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1182 _mm_maskz_reduce_sd (__mmask8 __U, __m128d __A, __m128d __B, int __C)
1184 return (__m128d) __builtin_ia32_reducesd_mask ((__v2df) __A,
1186 (__v2df) _mm_setzero_pd (),
1190 extern __inline __m128
1191 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1192 _mm_reduce_ss (__m128 __A, __m128 __B, int __C)
1194 return (__m128) __builtin_ia32_reducess_mask ((__v4sf) __A,
1196 (__v4sf) _mm_setzero_ps (),
1201 extern __inline __m128
1202 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1203 _mm_mask_reduce_ss (__m128 __W, __mmask8 __U, __m128 __A,
1204 __m128 __B, int __C)
1206 return (__m128) __builtin_ia32_reducess_mask ((__v4sf) __A,
1212 extern __inline __m128
1213 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1214 _mm_maskz_reduce_ss (__mmask8 __U, __m128 __A, __m128 __B, int __C)
1216 return (__m128) __builtin_ia32_reducess_mask ((__v4sf) __A,
1218 (__v4sf) _mm_setzero_ps (),
1222 extern __inline __m128d
1223 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1224 _mm_range_sd (__m128d __A, __m128d __B, int __C)
1226 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1231 _MM_FROUND_CUR_DIRECTION);
1234 extern __inline __m128d
1235 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1236 _mm_mask_range_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B, int __C)
1238 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1242 _MM_FROUND_CUR_DIRECTION);
1245 extern __inline __m128d
1246 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1247 _mm_maskz_range_sd (__mmask8 __U, __m128d __A, __m128d __B, int __C)
1249 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1254 _MM_FROUND_CUR_DIRECTION);
1257 extern __inline __m128
1258 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1259 _mm_range_ss (__m128 __A, __m128 __B, int __C)
1261 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1266 _MM_FROUND_CUR_DIRECTION);
1269 extern __inline __m128
1270 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1271 _mm_mask_range_ss (__m128 __W, __mmask8 __U, __m128 __A, __m128 __B, int __C)
1273 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1277 _MM_FROUND_CUR_DIRECTION);
1281 extern __inline __m128
1282 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1283 _mm_maskz_range_ss (__mmask8 __U, __m128 __A, __m128 __B, int __C)
1285 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1290 _MM_FROUND_CUR_DIRECTION);
1293 extern __inline __m128d
1294 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1295 _mm_range_round_sd (__m128d __A, __m128d __B, int __C, const int __R)
1297 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1301 (__mmask8) -1, __R);
1304 extern __inline __m128d
1305 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1306 _mm_mask_range_round_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B,
1307 int __C, const int __R)
1309 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1312 (__mmask8) __U, __R);
1315 extern __inline __m128d
1316 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1317 _mm_maskz_range_round_sd (__mmask8 __U, __m128d __A, __m128d __B, int __C,
1320 return (__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df) __A,
1324 (__mmask8) __U, __R);
1327 extern __inline __m128
1328 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1329 _mm_range_round_ss (__m128 __A, __m128 __B, int __C, const int __R)
1331 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1335 (__mmask8) -1, __R);
1338 extern __inline __m128
1339 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1340 _mm_mask_range_round_ss (__m128 __W, __mmask8 __U, __m128 __A, __m128 __B,
1341 int __C, const int __R)
1343 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1346 (__mmask8) __U, __R);
1349 extern __inline __m128
1350 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1351 _mm_maskz_range_round_ss (__mmask8 __U, __m128 __A, __m128 __B, int __C,
1354 return (__m128) __builtin_ia32_rangess128_mask_round ((__v4sf) __A,
1358 (__mmask8) __U, __R);
1361 extern __inline __mmask8
1362 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1363 _mm_fpclass_ss_mask (__m128 __A, const int __imm)
1365 return (__mmask8) __builtin_ia32_fpclassss ((__v4sf) __A, __imm);
1368 extern __inline __mmask8
1369 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1370 _mm_fpclass_sd_mask (__m128d __A, const int __imm)
1372 return (__mmask8) __builtin_ia32_fpclasssd ((__v2df) __A, __imm);
1375 extern __inline __m512i
1376 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1377 _mm512_cvtt_roundpd_epi64 (__m512d __A, const int __R)
1379 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
1381 _mm512_setzero_si512 (),
1386 extern __inline __m512i
1387 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1388 _mm512_mask_cvtt_roundpd_epi64 (__m512i __W, __mmask8 __U, __m512d __A,
1391 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
1397 extern __inline __m512i
1398 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1399 _mm512_maskz_cvtt_roundpd_epi64 (__mmask8 __U, __m512d __A,
1402 return (__m512i) __builtin_ia32_cvttpd2qq512_mask ((__v8df) __A,
1404 _mm512_setzero_si512 (),
1409 extern __inline __m512i
1410 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1411 _mm512_cvtt_roundpd_epu64 (__m512d __A, const int __R)
1413 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
1415 _mm512_setzero_si512 (),
1420 extern __inline __m512i
1421 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1422 _mm512_mask_cvtt_roundpd_epu64 (__m512i __W, __mmask8 __U, __m512d __A,
1425 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
1431 extern __inline __m512i
1432 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1433 _mm512_maskz_cvtt_roundpd_epu64 (__mmask8 __U, __m512d __A,
1436 return (__m512i) __builtin_ia32_cvttpd2uqq512_mask ((__v8df) __A,
1438 _mm512_setzero_si512 (),
1443 extern __inline __m512i
1444 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1445 _mm512_cvtt_roundps_epi64 (__m256 __A, const int __R)
1447 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
1449 _mm512_setzero_si512 (),
1454 extern __inline __m512i
1455 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1456 _mm512_mask_cvtt_roundps_epi64 (__m512i __W, __mmask8 __U, __m256 __A,
1459 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
1465 extern __inline __m512i
1466 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1467 _mm512_maskz_cvtt_roundps_epi64 (__mmask8 __U, __m256 __A,
1470 return (__m512i) __builtin_ia32_cvttps2qq512_mask ((__v8sf) __A,
1472 _mm512_setzero_si512 (),
1477 extern __inline __m512i
1478 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1479 _mm512_cvtt_roundps_epu64 (__m256 __A, const int __R)
1481 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
1483 _mm512_setzero_si512 (),
1488 extern __inline __m512i
1489 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1490 _mm512_mask_cvtt_roundps_epu64 (__m512i __W, __mmask8 __U, __m256 __A,
1493 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
1499 extern __inline __m512i
1500 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1501 _mm512_maskz_cvtt_roundps_epu64 (__mmask8 __U, __m256 __A,
1504 return (__m512i) __builtin_ia32_cvttps2uqq512_mask ((__v8sf) __A,
1506 _mm512_setzero_si512 (),
1511 extern __inline __m512i
1512 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1513 _mm512_cvt_roundpd_epi64 (__m512d __A, const int __R)
1515 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
1517 _mm512_setzero_si512 (),
1522 extern __inline __m512i
1523 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1524 _mm512_mask_cvt_roundpd_epi64 (__m512i __W, __mmask8 __U, __m512d __A,
1527 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
1533 extern __inline __m512i
1534 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1535 _mm512_maskz_cvt_roundpd_epi64 (__mmask8 __U, __m512d __A,
1538 return (__m512i) __builtin_ia32_cvtpd2qq512_mask ((__v8df) __A,
1540 _mm512_setzero_si512 (),
1545 extern __inline __m512i
1546 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1547 _mm512_cvt_roundpd_epu64 (__m512d __A, const int __R)
1549 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
1551 _mm512_setzero_si512 (),
1556 extern __inline __m512i
1557 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1558 _mm512_mask_cvt_roundpd_epu64 (__m512i __W, __mmask8 __U, __m512d __A,
1561 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
1567 extern __inline __m512i
1568 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1569 _mm512_maskz_cvt_roundpd_epu64 (__mmask8 __U, __m512d __A,
1572 return (__m512i) __builtin_ia32_cvtpd2uqq512_mask ((__v8df) __A,
1574 _mm512_setzero_si512 (),
1579 extern __inline __m512i
1580 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1581 _mm512_cvt_roundps_epi64 (__m256 __A, const int __R)
1583 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
1585 _mm512_setzero_si512 (),
1590 extern __inline __m512i
1591 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1592 _mm512_mask_cvt_roundps_epi64 (__m512i __W, __mmask8 __U, __m256 __A,
1595 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
1601 extern __inline __m512i
1602 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1603 _mm512_maskz_cvt_roundps_epi64 (__mmask8 __U, __m256 __A,
1606 return (__m512i) __builtin_ia32_cvtps2qq512_mask ((__v8sf) __A,
1608 _mm512_setzero_si512 (),
1613 extern __inline __m512i
1614 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1615 _mm512_cvt_roundps_epu64 (__m256 __A, const int __R)
1617 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
1619 _mm512_setzero_si512 (),
1624 extern __inline __m512i
1625 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1626 _mm512_mask_cvt_roundps_epu64 (__m512i __W, __mmask8 __U, __m256 __A,
1629 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
1635 extern __inline __m512i
1636 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1637 _mm512_maskz_cvt_roundps_epu64 (__mmask8 __U, __m256 __A,
1640 return (__m512i) __builtin_ia32_cvtps2uqq512_mask ((__v8sf) __A,
1642 _mm512_setzero_si512 (),
1647 extern __inline __m256
1648 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1649 _mm512_cvt_roundepi64_ps (__m512i __A, const int __R)
1651 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
1653 _mm256_setzero_ps (),
1658 extern __inline __m256
1659 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1660 _mm512_mask_cvt_roundepi64_ps (__m256 __W, __mmask8 __U, __m512i __A,
1663 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
1669 extern __inline __m256
1670 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1671 _mm512_maskz_cvt_roundepi64_ps (__mmask8 __U, __m512i __A,
1674 return (__m256) __builtin_ia32_cvtqq2ps512_mask ((__v8di) __A,
1676 _mm256_setzero_ps (),
1681 extern __inline __m256
1682 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1683 _mm512_cvt_roundepu64_ps (__m512i __A, const int __R)
1685 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
1687 _mm256_setzero_ps (),
1692 extern __inline __m256
1693 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1694 _mm512_mask_cvt_roundepu64_ps (__m256 __W, __mmask8 __U, __m512i __A,
1697 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
1703 extern __inline __m256
1704 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1705 _mm512_maskz_cvt_roundepu64_ps (__mmask8 __U, __m512i __A,
1708 return (__m256) __builtin_ia32_cvtuqq2ps512_mask ((__v8di) __A,
1710 _mm256_setzero_ps (),
1715 extern __inline __m512d
1716 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1717 _mm512_cvt_roundepi64_pd (__m512i __A, const int __R)
1719 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1721 _mm512_setzero_pd (),
1726 extern __inline __m512d
1727 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1728 _mm512_mask_cvt_roundepi64_pd (__m512d __W, __mmask8 __U, __m512i __A,
1731 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1737 extern __inline __m512d
1738 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1739 _mm512_maskz_cvt_roundepi64_pd (__mmask8 __U, __m512i __A,
1742 return (__m512d) __builtin_ia32_cvtqq2pd512_mask ((__v8di) __A,
1744 _mm512_setzero_pd (),
1749 extern __inline __m512d
1750 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1751 _mm512_cvt_roundepu64_pd (__m512i __A, const int __R)
1753 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1755 _mm512_setzero_pd (),
1760 extern __inline __m512d
1761 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1762 _mm512_mask_cvt_roundepu64_pd (__m512d __W, __mmask8 __U, __m512i __A,
1765 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1771 extern __inline __m512d
1772 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1773 _mm512_maskz_cvt_roundepu64_pd (__mmask8 __U, __m512i __A,
1776 return (__m512d) __builtin_ia32_cvtuqq2pd512_mask ((__v8di) __A,
1778 _mm512_setzero_pd (),
1783 extern __inline __m512d
1784 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1785 _mm512_reduce_pd (__m512d __A, int __B)
1787 return (__m512d) __builtin_ia32_reducepd512_mask ((__v8df) __A, __B,
1789 _mm512_setzero_pd (),
1793 extern __inline __m512d
1794 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1795 _mm512_mask_reduce_pd (__m512d __W, __mmask8 __U, __m512d __A, int __B)
1797 return (__m512d) __builtin_ia32_reducepd512_mask ((__v8df) __A, __B,
1802 extern __inline __m512d
1803 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1804 _mm512_maskz_reduce_pd (__mmask8 __U, __m512d __A, int __B)
1806 return (__m512d) __builtin_ia32_reducepd512_mask ((__v8df) __A, __B,
1808 _mm512_setzero_pd (),
1812 extern __inline __m512
1813 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1814 _mm512_reduce_ps (__m512 __A, int __B)
1816 return (__m512) __builtin_ia32_reduceps512_mask ((__v16sf) __A, __B,
1818 _mm512_setzero_ps (),
1822 extern __inline __m512
1823 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1824 _mm512_mask_reduce_ps (__m512 __W, __mmask16 __U, __m512 __A, int __B)
1826 return (__m512) __builtin_ia32_reduceps512_mask ((__v16sf) __A, __B,
1831 extern __inline __m512
1832 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1833 _mm512_maskz_reduce_ps (__mmask16 __U, __m512 __A, int __B)
1835 return (__m512) __builtin_ia32_reduceps512_mask ((__v16sf) __A, __B,
1837 _mm512_setzero_ps (),
1841 extern __inline __m256
1842 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1843 _mm512_extractf32x8_ps (__m512 __A, const int __imm)
1845 return (__m256) __builtin_ia32_extractf32x8_mask ((__v16sf) __A,
1848 _mm256_setzero_ps (),
1852 extern __inline __m256
1853 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1854 _mm512_mask_extractf32x8_ps (__m256 __W, __mmask8 __U, __m512 __A,
1857 return (__m256) __builtin_ia32_extractf32x8_mask ((__v16sf) __A,
1863 extern __inline __m256
1864 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1865 _mm512_maskz_extractf32x8_ps (__mmask8 __U, __m512 __A,
1868 return (__m256) __builtin_ia32_extractf32x8_mask ((__v16sf) __A,
1871 _mm256_setzero_ps (),
1875 extern __inline __m128d
1876 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1877 _mm512_extractf64x2_pd (__m512d __A, const int __imm)
1879 return (__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df) __A,
1886 extern __inline __m128d
1887 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1888 _mm512_mask_extractf64x2_pd (__m128d __W, __mmask8 __U, __m512d __A,
1891 return (__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df) __A,
1898 extern __inline __m128d
1899 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1900 _mm512_maskz_extractf64x2_pd (__mmask8 __U, __m512d __A,
1903 return (__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df) __A,
1911 extern __inline __m256i
1912 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1913 _mm512_extracti32x8_epi32 (__m512i __A, const int __imm)
1915 return (__m256i) __builtin_ia32_extracti32x8_mask ((__v16si) __A,
1918 _mm256_setzero_si256 (),
1922 extern __inline __m256i
1923 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1924 _mm512_mask_extracti32x8_epi32 (__m256i __W, __mmask8 __U, __m512i __A,
1927 return (__m256i) __builtin_ia32_extracti32x8_mask ((__v16si) __A,
1933 extern __inline __m256i
1934 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1935 _mm512_maskz_extracti32x8_epi32 (__mmask8 __U, __m512i __A,
1938 return (__m256i) __builtin_ia32_extracti32x8_mask ((__v16si) __A,
1941 _mm256_setzero_si256 (),
1945 extern __inline __m128i
1946 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1947 _mm512_extracti64x2_epi64 (__m512i __A, const int __imm)
1949 return (__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di) __A,
1952 _mm_setzero_si128 (),
1956 extern __inline __m128i
1957 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1958 _mm512_mask_extracti64x2_epi64 (__m128i __W, __mmask8 __U, __m512i __A,
1961 return (__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di) __A,
1968 extern __inline __m128i
1969 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1970 _mm512_maskz_extracti64x2_epi64 (__mmask8 __U, __m512i __A,
1973 return (__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di) __A,
1976 _mm_setzero_si128 (),
1981 extern __inline __m512d
1982 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1983 _mm512_range_round_pd (__m512d __A, __m512d __B, int __C,
1986 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
1989 _mm512_setzero_pd (),
1994 extern __inline __m512d
1995 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
1996 _mm512_mask_range_round_pd (__m512d __W, __mmask8 __U,
1997 __m512d __A, __m512d __B, int __C,
2000 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
2007 extern __inline __m512d
2008 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2009 _mm512_maskz_range_round_pd (__mmask8 __U, __m512d __A, __m512d __B,
2010 int __C, const int __R)
2012 return (__m512d) __builtin_ia32_rangepd512_mask ((__v8df) __A,
2015 _mm512_setzero_pd (),
2020 extern __inline __m512
2021 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2022 _mm512_range_round_ps (__m512 __A, __m512 __B, int __C, const int __R)
2024 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
2027 _mm512_setzero_ps (),
2032 extern __inline __m512
2033 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2034 _mm512_mask_range_round_ps (__m512 __W, __mmask16 __U,
2035 __m512 __A, __m512 __B, int __C,
2038 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
2045 extern __inline __m512
2046 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2047 _mm512_maskz_range_round_ps (__mmask16 __U, __m512 __A, __m512 __B,
2048 int __C, const int __R)
2050 return (__m512) __builtin_ia32_rangeps512_mask ((__v16sf) __A,
2053 _mm512_setzero_ps (),
2058 extern __inline __m512i
2059 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2060 _mm512_inserti32x8 (__m512i __A, __m256i __B, const int __imm)
2062 return (__m512i) __builtin_ia32_inserti32x8_mask ((__v16si) __A,
2066 _mm512_setzero_si512 (),
2070 extern __inline __m512i
2071 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2072 _mm512_mask_inserti32x8 (__m512i __W, __mmask16 __U, __m512i __A,
2073 __m256i __B, const int __imm)
2075 return (__m512i) __builtin_ia32_inserti32x8_mask ((__v16si) __A,
2082 extern __inline __m512i
2083 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2084 _mm512_maskz_inserti32x8 (__mmask16 __U, __m512i __A, __m256i __B,
2087 return (__m512i) __builtin_ia32_inserti32x8_mask ((__v16si) __A,
2091 _mm512_setzero_si512 (),
2095 extern __inline __m512
2096 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2097 _mm512_insertf32x8 (__m512 __A, __m256 __B, const int __imm)
2099 return (__m512) __builtin_ia32_insertf32x8_mask ((__v16sf) __A,
2103 _mm512_setzero_ps (),
2107 extern __inline __m512
2108 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2109 _mm512_mask_insertf32x8 (__m512 __W, __mmask16 __U, __m512 __A,
2110 __m256 __B, const int __imm)
2112 return (__m512) __builtin_ia32_insertf32x8_mask ((__v16sf) __A,
2119 extern __inline __m512
2120 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2121 _mm512_maskz_insertf32x8 (__mmask16 __U, __m512 __A, __m256 __B,
2124 return (__m512) __builtin_ia32_insertf32x8_mask ((__v16sf) __A,
2128 _mm512_setzero_ps (),
2132 extern __inline __m512i
2133 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2134 _mm512_inserti64x2 (__m512i __A, __m128i __B, const int __imm)
2136 return (__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di) __A,
2140 _mm512_setzero_si512 (),
2144 extern __inline __m512i
2145 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2146 _mm512_mask_inserti64x2 (__m512i __W, __mmask8 __U, __m512i __A,
2147 __m128i __B, const int __imm)
2149 return (__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di) __A,
2157 extern __inline __m512i
2158 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2159 _mm512_maskz_inserti64x2 (__mmask8 __U, __m512i __A, __m128i __B,
2162 return (__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di) __A,
2166 _mm512_setzero_si512 (),
2171 extern __inline __m512d
2172 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2173 _mm512_insertf64x2 (__m512d __A, __m128d __B, const int __imm)
2175 return (__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df) __A,
2179 _mm512_setzero_pd (),
2183 extern __inline __m512d
2184 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2185 _mm512_mask_insertf64x2 (__m512d __W, __mmask8 __U, __m512d __A,
2186 __m128d __B, const int __imm)
2188 return (__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df) __A,
2196 extern __inline __m512d
2197 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2198 _mm512_maskz_insertf64x2 (__mmask8 __U, __m512d __A, __m128d __B,
2201 return (__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df) __A,
2205 _mm512_setzero_pd (),
2210 extern __inline __mmask8
2211 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2212 _mm512_mask_fpclass_pd_mask (__mmask8 __U, __m512d __A,
2215 return (__mmask8) __builtin_ia32_fpclasspd512_mask ((__v8df) __A,
2219 extern __inline __mmask8
2220 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2221 _mm512_fpclass_pd_mask (__m512d __A, const int __imm)
2223 return (__mmask8) __builtin_ia32_fpclasspd512_mask ((__v8df) __A,
2228 extern __inline __mmask16
2229 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2230 _mm512_mask_fpclass_ps_mask (__mmask16 __U, __m512 __A,
2233 return (__mmask16) __builtin_ia32_fpclassps512_mask ((__v16sf) __A,
2237 extern __inline __mmask16
2238 __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
2239 _mm512_fpclass_ps_mask (__m512 __A, const int __imm)
2241 return (__mmask16) __builtin_ia32_fpclassps512_mask ((__v16sf) __A,
2247 #define _kshiftli_mask8(X, Y) \
2248 ((__mmask8) __builtin_ia32_kshiftliqi ((__mmask8)(X), (__mmask8)(Y)))
2250 #define _kshiftri_mask8(X, Y) \
2251 ((__mmask8) __builtin_ia32_kshiftriqi ((__mmask8)(X), (__mmask8)(Y)))
2253 #define _mm_range_sd(A, B, C) \
2254 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2255 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2256 (__mmask8) -1, _MM_FROUND_CUR_DIRECTION))
2258 #define _mm_mask_range_sd(W, U, A, B, C) \
2259 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2260 (__v2df)(__m128d)(B), (int)(C), (__v2df)(__m128d)(W), \
2261 (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2263 #define _mm_maskz_range_sd(U, A, B, C) \
2264 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2265 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2266 (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2268 #define _mm_range_ss(A, B, C) \
2269 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2270 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2271 (__mmask8) -1, _MM_FROUND_CUR_DIRECTION))
2273 #define _mm_mask_range_ss(W, U, A, B, C) \
2274 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2275 (__v4sf)(__m128)(B), (int)(C), (__v4sf)(__m128)(W), \
2276 (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2278 #define _mm_maskz_range_ss(U, A, B, C) \
2279 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2280 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2281 (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2283 #define _mm_range_round_sd(A, B, C, R) \
2284 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2285 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2286 (__mmask8) -1, (R)))
2288 #define _mm_mask_range_round_sd(W, U, A, B, C, R) \
2289 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2290 (__v2df)(__m128d)(B), (int)(C), (__v2df)(__m128d)(W), \
2291 (__mmask8)(U), (R)))
2293 #define _mm_maskz_range_round_sd(U, A, B, C, R) \
2294 ((__m128d) __builtin_ia32_rangesd128_mask_round ((__v2df)(__m128d)(A), \
2295 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2296 (__mmask8)(U), (R)))
2298 #define _mm_range_round_ss(A, B, C, R) \
2299 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2300 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2301 (__mmask8) -1, (R)))
2303 #define _mm_mask_range_round_ss(W, U, A, B, C, R) \
2304 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2305 (__v4sf)(__m128)(B), (int)(C), (__v4sf)(__m128)(W), \
2306 (__mmask8)(U), (R)))
2308 #define _mm_maskz_range_round_ss(U, A, B, C, R) \
2309 ((__m128) __builtin_ia32_rangess128_mask_round ((__v4sf)(__m128)(A), \
2310 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2311 (__mmask8)(U), (R)))
2313 #define _mm512_cvtt_roundpd_epi64(A, B) \
2314 ((__m512i)__builtin_ia32_cvttpd2qq512_mask ((A), (__v8di) \
2315 _mm512_setzero_si512 (), \
2318 #define _mm512_mask_cvtt_roundpd_epi64(W, U, A, B) \
2319 ((__m512i)__builtin_ia32_cvttpd2qq512_mask ((A), (__v8di)(W), (U), (B)))
2321 #define _mm512_maskz_cvtt_roundpd_epi64(U, A, B) \
2322 ((__m512i)__builtin_ia32_cvttpd2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2324 #define _mm512_cvtt_roundpd_epu64(A, B) \
2325 ((__m512i)__builtin_ia32_cvttpd2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2327 #define _mm512_mask_cvtt_roundpd_epu64(W, U, A, B) \
2328 ((__m512i)__builtin_ia32_cvttpd2uqq512_mask ((A), (__v8di)(W), (U), (B)))
2330 #define _mm512_maskz_cvtt_roundpd_epu64(U, A, B) \
2331 ((__m512i)__builtin_ia32_cvttpd2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2333 #define _mm512_cvtt_roundps_epi64(A, B) \
2334 ((__m512i)__builtin_ia32_cvttps2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2336 #define _mm512_mask_cvtt_roundps_epi64(W, U, A, B) \
2337 ((__m512i)__builtin_ia32_cvttps2qq512_mask ((A), (__v8di)(W), (U), (B)))
2339 #define _mm512_maskz_cvtt_roundps_epi64(U, A, B) \
2340 ((__m512i)__builtin_ia32_cvttps2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2342 #define _mm512_cvtt_roundps_epu64(A, B) \
2343 ((__m512i)__builtin_ia32_cvttps2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2345 #define _mm512_mask_cvtt_roundps_epu64(W, U, A, B) \
2346 ((__m512i)__builtin_ia32_cvttps2uqq512_mask ((A), (__v8di)(W), (U), (B)))
2348 #define _mm512_maskz_cvtt_roundps_epu64(U, A, B) \
2349 ((__m512i)__builtin_ia32_cvttps2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2351 #define _mm512_cvt_roundpd_epi64(A, B) \
2352 ((__m512i)__builtin_ia32_cvtpd2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2354 #define _mm512_mask_cvt_roundpd_epi64(W, U, A, B) \
2355 ((__m512i)__builtin_ia32_cvtpd2qq512_mask ((A), (__v8di)(W), (U), (B)))
2357 #define _mm512_maskz_cvt_roundpd_epi64(U, A, B) \
2358 ((__m512i)__builtin_ia32_cvtpd2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2360 #define _mm512_cvt_roundpd_epu64(A, B) \
2361 ((__m512i)__builtin_ia32_cvtpd2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2363 #define _mm512_mask_cvt_roundpd_epu64(W, U, A, B) \
2364 ((__m512i)__builtin_ia32_cvtpd2uqq512_mask ((A), (__v8di)(W), (U), (B)))
2366 #define _mm512_maskz_cvt_roundpd_epu64(U, A, B) \
2367 ((__m512i)__builtin_ia32_cvtpd2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2369 #define _mm512_cvt_roundps_epi64(A, B) \
2370 ((__m512i)__builtin_ia32_cvtps2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2372 #define _mm512_mask_cvt_roundps_epi64(W, U, A, B) \
2373 ((__m512i)__builtin_ia32_cvtps2qq512_mask ((A), (__v8di)(W), (U), (B)))
2375 #define _mm512_maskz_cvt_roundps_epi64(U, A, B) \
2376 ((__m512i)__builtin_ia32_cvtps2qq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2378 #define _mm512_cvt_roundps_epu64(A, B) \
2379 ((__m512i)__builtin_ia32_cvtps2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), -1, (B)))
2381 #define _mm512_mask_cvt_roundps_epu64(W, U, A, B) \
2382 ((__m512i)__builtin_ia32_cvtps2uqq512_mask ((A), (__v8di)(W), (U), (B)))
2384 #define _mm512_maskz_cvt_roundps_epu64(U, A, B) \
2385 ((__m512i)__builtin_ia32_cvtps2uqq512_mask ((A), (__v8di)_mm512_setzero_si512 (), (U), (B)))
2387 #define _mm512_cvt_roundepi64_ps(A, B) \
2388 ((__m256)__builtin_ia32_cvtqq2ps512_mask ((__v8di)(A), (__v8sf)_mm256_setzero_ps (), -1, (B)))
2390 #define _mm512_mask_cvt_roundepi64_ps(W, U, A, B) \
2391 ((__m256)__builtin_ia32_cvtqq2ps512_mask ((__v8di)(A), (W), (U), (B)))
2393 #define _mm512_maskz_cvt_roundepi64_ps(U, A, B) \
2394 ((__m256)__builtin_ia32_cvtqq2ps512_mask ((__v8di)(A), (__v8sf)_mm256_setzero_ps (), (U), (B)))
2396 #define _mm512_cvt_roundepu64_ps(A, B) \
2397 ((__m256)__builtin_ia32_cvtuqq2ps512_mask ((__v8di)(A), (__v8sf)_mm256_setzero_ps (), -1, (B)))
2399 #define _mm512_mask_cvt_roundepu64_ps(W, U, A, B) \
2400 ((__m256)__builtin_ia32_cvtuqq2ps512_mask ((__v8di)(A), (W), (U), (B)))
2402 #define _mm512_maskz_cvt_roundepu64_ps(U, A, B) \
2403 ((__m256)__builtin_ia32_cvtuqq2ps512_mask ((__v8di)(A), (__v8sf)_mm256_setzero_ps (), (U), (B)))
2405 #define _mm512_cvt_roundepi64_pd(A, B) \
2406 ((__m512d)__builtin_ia32_cvtqq2pd512_mask ((__v8di)(A), (__v8df)_mm512_setzero_pd (), -1, (B)))
2408 #define _mm512_mask_cvt_roundepi64_pd(W, U, A, B) \
2409 ((__m512d)__builtin_ia32_cvtqq2pd512_mask ((__v8di)(A), (W), (U), (B)))
2411 #define _mm512_maskz_cvt_roundepi64_pd(U, A, B) \
2412 ((__m512d)__builtin_ia32_cvtqq2pd512_mask ((__v8di)(A), (__v8df)_mm512_setzero_pd (), (U), (B)))
2414 #define _mm512_cvt_roundepu64_pd(A, B) \
2415 ((__m512d)__builtin_ia32_cvtuqq2pd512_mask ((__v8di)(A), (__v8df)_mm512_setzero_pd (), -1, (B)))
2417 #define _mm512_mask_cvt_roundepu64_pd(W, U, A, B) \
2418 ((__m512d)__builtin_ia32_cvtuqq2pd512_mask ((__v8di)(A), (W), (U), (B)))
2420 #define _mm512_maskz_cvt_roundepu64_pd(U, A, B) \
2421 ((__m512d)__builtin_ia32_cvtuqq2pd512_mask ((__v8di)(A), (__v8df)_mm512_setzero_pd (), (U), (B)))
2423 #define _mm512_reduce_pd(A, B) \
2424 ((__m512d) __builtin_ia32_reducepd512_mask ((__v8df)(__m512d)(A), \
2425 (int)(B), (__v8df)_mm512_setzero_pd (), (__mmask8)-1))
2427 #define _mm512_mask_reduce_pd(W, U, A, B) \
2428 ((__m512d) __builtin_ia32_reducepd512_mask ((__v8df)(__m512d)(A), \
2429 (int)(B), (__v8df)(__m512d)(W), (__mmask8)(U)))
2431 #define _mm512_maskz_reduce_pd(U, A, B) \
2432 ((__m512d) __builtin_ia32_reducepd512_mask ((__v8df)(__m512d)(A), \
2433 (int)(B), (__v8df)_mm512_setzero_pd (), (__mmask8)(U)))
2435 #define _mm512_reduce_ps(A, B) \
2436 ((__m512) __builtin_ia32_reduceps512_mask ((__v16sf)(__m512)(A), \
2437 (int)(B), (__v16sf)_mm512_setzero_ps (), (__mmask16)-1))
2439 #define _mm512_mask_reduce_ps(W, U, A, B) \
2440 ((__m512) __builtin_ia32_reduceps512_mask ((__v16sf)(__m512)(A), \
2441 (int)(B), (__v16sf)(__m512)(W), (__mmask16)(U)))
2443 #define _mm512_maskz_reduce_ps(U, A, B) \
2444 ((__m512) __builtin_ia32_reduceps512_mask ((__v16sf)(__m512)(A), \
2445 (int)(B), (__v16sf)_mm512_setzero_ps (), (__mmask16)(U)))
2447 #define _mm512_extractf32x8_ps(X, C) \
2448 ((__m256) __builtin_ia32_extractf32x8_mask ((__v16sf)(__m512) (X), \
2449 (int) (C), (__v8sf)(__m256) _mm256_setzero_ps (), (__mmask8)-1))
2451 #define _mm512_mask_extractf32x8_ps(W, U, X, C) \
2452 ((__m256) __builtin_ia32_extractf32x8_mask ((__v16sf)(__m512) (X), \
2453 (int) (C), (__v8sf)(__m256) (W), (__mmask8) (U)))
2455 #define _mm512_maskz_extractf32x8_ps(U, X, C) \
2456 ((__m256) __builtin_ia32_extractf32x8_mask ((__v16sf)(__m512) (X), \
2457 (int) (C), (__v8sf)(__m256) _mm256_setzero_ps (), (__mmask8) (U)))
2459 #define _mm512_extractf64x2_pd(X, C) \
2460 ((__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df)(__m512d) (X),\
2461 (int) (C), (__v2df)(__m128d) _mm_setzero_pd (), (__mmask8)-1))
2463 #define _mm512_mask_extractf64x2_pd(W, U, X, C) \
2464 ((__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df)(__m512d) (X),\
2465 (int) (C), (__v2df)(__m128d) (W), (__mmask8) (U)))
2467 #define _mm512_maskz_extractf64x2_pd(U, X, C) \
2468 ((__m128d) __builtin_ia32_extractf64x2_512_mask ((__v8df)(__m512d) (X),\
2469 (int) (C), (__v2df)(__m128d) _mm_setzero_pd (), (__mmask8) (U)))
2471 #define _mm512_extracti32x8_epi32(X, C) \
2472 ((__m256i) __builtin_ia32_extracti32x8_mask ((__v16si)(__m512i) (X), \
2473 (int) (C), (__v8si)(__m256i) _mm256_setzero_si256 (), (__mmask8)-1))
2475 #define _mm512_mask_extracti32x8_epi32(W, U, X, C) \
2476 ((__m256i) __builtin_ia32_extracti32x8_mask ((__v16si)(__m512i) (X), \
2477 (int) (C), (__v8si)(__m256i) (W), (__mmask8) (U)))
2479 #define _mm512_maskz_extracti32x8_epi32(U, X, C) \
2480 ((__m256i) __builtin_ia32_extracti32x8_mask ((__v16si)(__m512i) (X), \
2481 (int) (C), (__v8si)(__m256i) _mm256_setzero_si256 (), (__mmask8) (U)))
2483 #define _mm512_extracti64x2_epi64(X, C) \
2484 ((__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di)(__m512i) (X),\
2485 (int) (C), (__v2di)(__m128i) _mm_setzero_si128 (), (__mmask8)-1))
2487 #define _mm512_mask_extracti64x2_epi64(W, U, X, C) \
2488 ((__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di)(__m512i) (X),\
2489 (int) (C), (__v2di)(__m128i) (W), (__mmask8) (U)))
2491 #define _mm512_maskz_extracti64x2_epi64(U, X, C) \
2492 ((__m128i) __builtin_ia32_extracti64x2_512_mask ((__v8di)(__m512i) (X),\
2493 (int) (C), (__v2di)(__m128i) _mm_setzero_si128 (), (__mmask8) (U)))
2495 #define _mm512_range_pd(A, B, C) \
2496 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2497 (__v8df)(__m512d)(B), (int)(C), \
2498 (__v8df)_mm512_setzero_pd (), (__mmask8)-1, _MM_FROUND_CUR_DIRECTION))
2500 #define _mm512_mask_range_pd(W, U, A, B, C) \
2501 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2502 (__v8df)(__m512d)(B), (int)(C), \
2503 (__v8df)(__m512d)(W), (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2505 #define _mm512_maskz_range_pd(U, A, B, C) \
2506 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2507 (__v8df)(__m512d)(B), (int)(C), \
2508 (__v8df)_mm512_setzero_pd (), (__mmask8)(U), _MM_FROUND_CUR_DIRECTION))
2510 #define _mm512_range_ps(A, B, C) \
2511 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2512 (__v16sf)(__m512)(B), (int)(C), \
2513 (__v16sf)_mm512_setzero_ps (), (__mmask16)-1, _MM_FROUND_CUR_DIRECTION))
2515 #define _mm512_mask_range_ps(W, U, A, B, C) \
2516 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2517 (__v16sf)(__m512)(B), (int)(C), \
2518 (__v16sf)(__m512)(W), (__mmask16)(U), _MM_FROUND_CUR_DIRECTION))
2520 #define _mm512_maskz_range_ps(U, A, B, C) \
2521 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2522 (__v16sf)(__m512)(B), (int)(C), \
2523 (__v16sf)_mm512_setzero_ps (), (__mmask16)(U), _MM_FROUND_CUR_DIRECTION))
2525 #define _mm512_range_round_pd(A, B, C, R) \
2526 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2527 (__v8df)(__m512d)(B), (int)(C), \
2528 (__v8df)_mm512_setzero_pd (), (__mmask8)-1, (R)))
2530 #define _mm512_mask_range_round_pd(W, U, A, B, C, R) \
2531 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2532 (__v8df)(__m512d)(B), (int)(C), \
2533 (__v8df)(__m512d)(W), (__mmask8)(U), (R)))
2535 #define _mm512_maskz_range_round_pd(U, A, B, C, R) \
2536 ((__m512d) __builtin_ia32_rangepd512_mask ((__v8df)(__m512d)(A), \
2537 (__v8df)(__m512d)(B), (int)(C), \
2538 (__v8df)_mm512_setzero_pd (), (__mmask8)(U), (R)))
2540 #define _mm512_range_round_ps(A, B, C, R) \
2541 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2542 (__v16sf)(__m512)(B), (int)(C), \
2543 (__v16sf)_mm512_setzero_ps (), (__mmask16)-1, (R)))
2545 #define _mm512_mask_range_round_ps(W, U, A, B, C, R) \
2546 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2547 (__v16sf)(__m512)(B), (int)(C), \
2548 (__v16sf)(__m512)(W), (__mmask16)(U), (R)))
2550 #define _mm512_maskz_range_round_ps(U, A, B, C, R) \
2551 ((__m512) __builtin_ia32_rangeps512_mask ((__v16sf)(__m512)(A), \
2552 (__v16sf)(__m512)(B), (int)(C), \
2553 (__v16sf)_mm512_setzero_ps (), (__mmask16)(U), (R)))
2555 #define _mm512_insertf64x2(X, Y, C) \
2556 ((__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df)(__m512d) (X),\
2557 (__v2df)(__m128d) (Y), (int) (C), (__v8df)(__m512d) (X), \
2560 #define _mm512_mask_insertf64x2(W, U, X, Y, C) \
2561 ((__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df)(__m512d) (X),\
2562 (__v2df)(__m128d) (Y), (int) (C), (__v8df)(__m512d) (W), \
2565 #define _mm512_maskz_insertf64x2(U, X, Y, C) \
2566 ((__m512d) __builtin_ia32_insertf64x2_512_mask ((__v8df)(__m512d) (X),\
2567 (__v2df)(__m128d) (Y), (int) (C), \
2568 (__v8df)(__m512d) _mm512_setzero_pd (), (__mmask8) (U)))
2570 #define _mm512_inserti64x2(X, Y, C) \
2571 ((__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di)(__m512i) (X),\
2572 (__v2di)(__m128i) (Y), (int) (C), (__v8di)(__m512i) (X), (__mmask8)-1))
2574 #define _mm512_mask_inserti64x2(W, U, X, Y, C) \
2575 ((__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di)(__m512i) (X),\
2576 (__v2di)(__m128i) (Y), (int) (C), (__v8di)(__m512i) (W), \
2579 #define _mm512_maskz_inserti64x2(U, X, Y, C) \
2580 ((__m512i) __builtin_ia32_inserti64x2_512_mask ((__v8di)(__m512i) (X),\
2581 (__v2di)(__m128i) (Y), (int) (C), \
2582 (__v8di)(__m512i) _mm512_setzero_si512 (), (__mmask8) (U)))
2584 #define _mm512_insertf32x8(X, Y, C) \
2585 ((__m512) __builtin_ia32_insertf32x8_mask ((__v16sf)(__m512) (X), \
2586 (__v8sf)(__m256) (Y), (int) (C),\
2587 (__v16sf)(__m512)_mm512_setzero_ps (),\
2590 #define _mm512_mask_insertf32x8(W, U, X, Y, C) \
2591 ((__m512) __builtin_ia32_insertf32x8_mask ((__v16sf)(__m512) (X), \
2592 (__v8sf)(__m256) (Y), (int) (C),\
2593 (__v16sf)(__m512)(W),\
2596 #define _mm512_maskz_insertf32x8(U, X, Y, C) \
2597 ((__m512) __builtin_ia32_insertf32x8_mask ((__v16sf)(__m512) (X), \
2598 (__v8sf)(__m256) (Y), (int) (C),\
2599 (__v16sf)(__m512)_mm512_setzero_ps (),\
2602 #define _mm512_inserti32x8(X, Y, C) \
2603 ((__m512i) __builtin_ia32_inserti32x8_mask ((__v16si)(__m512i) (X), \
2604 (__v8si)(__m256i) (Y), (int) (C),\
2605 (__v16si)(__m512i)_mm512_setzero_si512 (),\
2608 #define _mm512_mask_inserti32x8(W, U, X, Y, C) \
2609 ((__m512i) __builtin_ia32_inserti32x8_mask ((__v16si)(__m512i) (X), \
2610 (__v8si)(__m256i) (Y), (int) (C),\
2611 (__v16si)(__m512i)(W),\
2614 #define _mm512_maskz_inserti32x8(U, X, Y, C) \
2615 ((__m512i) __builtin_ia32_inserti32x8_mask ((__v16si)(__m512i) (X), \
2616 (__v8si)(__m256i) (Y), (int) (C),\
2617 (__v16si)(__m512i)_mm512_setzero_si512 (),\
2620 #define _mm_fpclass_ss_mask(X, C) \
2621 ((__mmask8) __builtin_ia32_fpclassss ((__v4sf) (__m128) (X), (int) (C))) \
2623 #define _mm_fpclass_sd_mask(X, C) \
2624 ((__mmask8) __builtin_ia32_fpclasssd ((__v2df) (__m128d) (X), (int) (C))) \
2626 #define _mm512_mask_fpclass_pd_mask(u, X, C) \
2627 ((__mmask8) __builtin_ia32_fpclasspd512_mask ((__v8df) (__m512d) (X), \
2628 (int) (C), (__mmask8)(u)))
2630 #define _mm512_mask_fpclass_ps_mask(u, x, c) \
2631 ((__mmask16) __builtin_ia32_fpclassps512_mask ((__v16sf) (__m512) (x),\
2632 (int) (c),(__mmask8)(u)))
2634 #define _mm512_fpclass_pd_mask(X, C) \
2635 ((__mmask8) __builtin_ia32_fpclasspd512_mask ((__v8df) (__m512d) (X), \
2636 (int) (C), (__mmask8)-1))
2638 #define _mm512_fpclass_ps_mask(x, c) \
2639 ((__mmask16) __builtin_ia32_fpclassps512_mask ((__v16sf) (__m512) (x),\
2640 (int) (c),(__mmask8)-1))
2642 #define _mm_reduce_sd(A, B, C) \
2643 ((__m128d) __builtin_ia32_reducesd_mask ((__v2df)(__m128d)(A), \
2644 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2647 #define _mm_mask_reduce_sd(W, U, A, B, C) \
2648 ((__m128d) __builtin_ia32_reducesd_mask ((__v2df)(__m128d)(A), \
2649 (__v2df)(__m128d)(B), (int)(C), (__v2df)(__m128d)(W), (__mmask8)(U)))
2651 #define _mm_maskz_reduce_sd(U, A, B, C) \
2652 ((__m128d) __builtin_ia32_reducesd_mask ((__v2df)(__m128d)(A), \
2653 (__v2df)(__m128d)(B), (int)(C), (__v2df) _mm_setzero_pd (), \
2656 #define _mm_reduce_ss(A, B, C) \
2657 ((__m128) __builtin_ia32_reducess_mask ((__v4sf)(__m128)(A), \
2658 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2661 #define _mm_mask_reduce_ss(W, U, A, B, C) \
2662 ((__m128) __builtin_ia32_reducess_mask ((__v4sf)(__m128)(A), \
2663 (__v4sf)(__m128)(B), (int)(C), (__v4sf)(__m128)(W), (__mmask8)(U)))
2665 #define _mm_maskz_reduce_ss(U, A, B, C) \
2666 ((__m128) __builtin_ia32_reducess_mask ((__v4sf)(__m128)(A), \
2667 (__v4sf)(__m128)(B), (int)(C), (__v4sf) _mm_setzero_ps (), \
2674 #ifdef __DISABLE_AVX512DQ__
2675 #undef __DISABLE_AVX512DQ__
2676 #pragma GCC pop_options
2677 #endif /* __DISABLE_AVX512DQ__ */
2679 #endif /* _AVX512DQINTRIN_H_INCLUDED */