18 typedef unsigned long long __mmask64;  typedef
30 static __inline __mmask64 __DEFAULT_FN_ATTRS
31 _knot_mask64(__mmask64 __M)  in _knot_mask64()
42 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
43 _kand_mask64(__mmask64 __A, __mmask64 __B)  in _kand_mask64()
45   return (__mmask64)__builtin_ia32_kanddi((__mmask64)__A, (__mmask64)__B);  in _kand_mask64()
54 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
55 _kandn_mask64(__mmask64 __A, __mmask64 __B)  in _kandn_mask64()
57   return (__mmask64)__builtin_ia32_kandndi((__mmask64)__A, (__mmask64)__B);  in _kandn_mask64()
66 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
67 _kor_mask64(__mmask64 __A, __mmask64 __B)  in _kor_mask64()
69   return (__mmask64)__builtin_ia32_kordi((__mmask64)__A, (__mmask64)__B);  in _kor_mask64()
78 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
79 _kxnor_mask64(__mmask64 __A, __mmask64 __B)  in _kxnor_mask64()
81   return (__mmask64)__builtin_ia32_kxnordi((__mmask64)__A, (__mmask64)__B);  in _kxnor_mask64()
90 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
91 _kxor_mask64(__mmask64 __A, __mmask64 __B)  in _kxor_mask64()
93   return (__mmask64)__builtin_ia32_kxordi((__mmask64)__A, (__mmask64)__B);  in _kxor_mask64()
115 _kortestc_mask64_u8(__mmask64 __A, __mmask64 __B)  in _kortestc_mask64_u8()
121 _kortestz_mask64_u8(__mmask64 __A, __mmask64 __B)  in _kortestz_mask64_u8()
127 _kortest_mask64_u8(__mmask64 __A, __mmask64 __B, unsigned char *__C) {  in _kortest_mask64_u8()
151 _ktestc_mask64_u8(__mmask64 __A, __mmask64 __B)  in _ktestc_mask64_u8()
157 _ktestz_mask64_u8(__mmask64 __A, __mmask64 __B)  in _ktestz_mask64_u8()
163 _ktest_mask64_u8(__mmask64 __A, __mmask64 __B, unsigned char *__C) {  in _ktest_mask64_u8()
174 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
175 _kadd_mask64(__mmask64 __A, __mmask64 __B)  in _kadd_mask64()
177   return (__mmask64)__builtin_ia32_kadddi((__mmask64)__A, (__mmask64)__B);  in _kadd_mask64()
187   (__mmask64)__builtin_ia32_kshiftlidi((__mmask64)(A), (unsigned int)(I))
190   (__mmask64)__builtin_ia32_kshiftridi((__mmask64)(A), (unsigned int)(I))
198 _cvtmask64_u64(__mmask64 __A) {  in _cvtmask64_u64()
199   return (unsigned long long)__builtin_ia32_kmovq((__mmask64)__A);  in _cvtmask64_u64()
207 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
209   return (__mmask64)__builtin_ia32_kmovq((__mmask64)__A);  in _cvtu64_mask64()
217 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
218 _load_mask64(__mmask64 *__A) {  in _load_mask64()
219   return (__mmask64)__builtin_ia32_kmovq(*(__mmask64 *)__A);  in _load_mask64()
228 _store_mask64(__mmask64 *__A, __mmask64 __B) {  in _store_mask64()
229   *(__mmask64 *)__A = __builtin_ia32_kmovq((__mmask64)__B);  in _store_mask64()
235   (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
237                                          (__mmask64)-1)
240   (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
242                                          (__mmask64)(m))
245   (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
247                                           (__mmask64)-1)
250   (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
252                                           (__mmask64)(m))
380 _mm512_mask_add_epi8(__m512i __W, __mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_mask_add_epi8()
381   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_add_epi8()
387 _mm512_maskz_add_epi8(__mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_maskz_add_epi8()
388   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_add_epi8()
399 _mm512_mask_sub_epi8(__m512i __W, __mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_mask_sub_epi8()
400   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_sub_epi8()
406 _mm512_maskz_sub_epi8(__mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_maskz_sub_epi8()
407   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_sub_epi8()
470 _mm512_mask_blend_epi8 (__mmask64 __U, __m512i __A, __m512i __W)  in _mm512_mask_blend_epi8()
472   return (__m512i) __builtin_ia32_selectb_512 ((__mmask64) __U,  in _mm512_mask_blend_epi8()
492 _mm512_mask_abs_epi8 (__m512i __W, __mmask64 __U, __m512i __A)  in _mm512_mask_abs_epi8()
494   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_abs_epi8()
500 _mm512_maskz_abs_epi8 (__mmask64 __U, __m512i __A)  in _mm512_maskz_abs_epi8()
502   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_abs_epi8()
558 _mm512_mask_packs_epi16(__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_packs_epi16()
560   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_packs_epi16()
566 _mm512_maskz_packs_epi16(__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_packs_epi16()
568   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_packs_epi16()
602 _mm512_mask_packus_epi16(__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_packus_epi16()
604   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_packus_epi16()
610 _mm512_maskz_packus_epi16(__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_packus_epi16()
612   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_packus_epi16()
624 _mm512_mask_adds_epi8 (__m512i __W, __mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_adds_epi8()
626   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_adds_epi8()
632 _mm512_maskz_adds_epi8 (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_adds_epi8()
634   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_adds_epi8()
668 _mm512_mask_adds_epu8 (__m512i __W, __mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_adds_epu8()
670   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_adds_epu8()
676 _mm512_maskz_adds_epu8 (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_adds_epu8()
678   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_adds_epu8()
712 _mm512_mask_avg_epu8 (__m512i __W, __mmask64 __U, __m512i __A,  in _mm512_mask_avg_epu8()
715   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_avg_epu8()
721 _mm512_maskz_avg_epu8 (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_avg_epu8()
723   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_avg_epu8()
758 _mm512_maskz_max_epi8 (__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_max_epi8()
760   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_max_epi8()
766 _mm512_mask_max_epi8 (__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_max_epi8()
768   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_max_epi8()
803 _mm512_maskz_max_epu8 (__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_max_epu8()
805   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_max_epu8()
811 _mm512_mask_max_epu8 (__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_max_epu8()
813   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_max_epu8()
847 _mm512_maskz_min_epi8 (__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_min_epi8()
849   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_min_epi8()
855 _mm512_mask_min_epi8 (__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_min_epi8()
857   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_min_epi8()
891 _mm512_maskz_min_epu8 (__mmask64 __M, __m512i __A, __m512i __B)  in _mm512_maskz_min_epu8()
893   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_maskz_min_epu8()
899 _mm512_mask_min_epu8 (__m512i __W, __mmask64 __M, __m512i __A, __m512i __B)  in _mm512_mask_min_epu8()
901   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__M,  in _mm512_mask_min_epu8()
935 _mm512_mask_shuffle_epi8(__m512i __W, __mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_shuffle_epi8()
937   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_shuffle_epi8()
943 _mm512_maskz_shuffle_epi8(__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_shuffle_epi8()
945   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_shuffle_epi8()
957 _mm512_mask_subs_epi8 (__m512i __W, __mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_subs_epi8()
959   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_subs_epi8()
965 _mm512_maskz_subs_epi8 (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_subs_epi8()
967   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_subs_epi8()
1001 _mm512_mask_subs_epu8 (__m512i __W, __mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_subs_epu8()
1003   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_subs_epu8()
1009 _mm512_maskz_subs_epu8 (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_maskz_subs_epu8()
1011   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_subs_epu8()
1281 _mm512_mask_unpackhi_epi8(__m512i __W, __mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_mask_unpackhi_epi8()
1282   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_unpackhi_epi8()
1288 _mm512_maskz_unpackhi_epi8(__mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_maskz_unpackhi_epi8()
1289   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_unpackhi_epi8()
1343 _mm512_mask_unpacklo_epi8(__m512i __W, __mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_mask_unpacklo_epi8()
1344   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_mask_unpacklo_epi8()
1350 _mm512_maskz_unpacklo_epi8(__mmask64 __U, __m512i __A, __m512i __B) {  in _mm512_maskz_unpacklo_epi8()
1351   return (__m512i)__builtin_ia32_selectb_512((__mmask64)__U,  in _mm512_maskz_unpacklo_epi8()
1686 _mm512_mask_mov_epi8 (__m512i __W, __mmask64 __U, __m512i __A)  in _mm512_mask_mov_epi8()
1688   return (__m512i) __builtin_ia32_selectb_512 ((__mmask64) __U,  in _mm512_mask_mov_epi8()
1694 _mm512_maskz_mov_epi8 (__mmask64 __U, __m512i __A)  in _mm512_maskz_mov_epi8()
1696   return (__m512i) __builtin_ia32_selectb_512 ((__mmask64) __U,  in _mm512_maskz_mov_epi8()
1702 _mm512_mask_set1_epi8 (__m512i __O, __mmask64 __M, char __A)  in _mm512_mask_set1_epi8()
1710 _mm512_maskz_set1_epi8 (__mmask64 __M, char __A)  in _mm512_maskz_set1_epi8()
1717 static __inline__ __mmask64 __DEFAULT_FN_ATTRS
1718 _mm512_kunpackd (__mmask64 __A, __mmask64 __B)  in _mm512_kunpackd()
1720   return (__mmask64) __builtin_ia32_kunpckdi ((__mmask64) __A,  in _mm512_kunpackd()
1721                 (__mmask64) __B);  in _mm512_kunpackd()
1767 _mm512_mask_loadu_epi8 (__m512i __W, __mmask64 __U, void const *__P)  in _mm512_mask_loadu_epi8()
1771                  (__mmask64) __U);  in _mm512_mask_loadu_epi8()
1775 _mm512_maskz_loadu_epi8 (__mmask64 __U, void const *__P)  in _mm512_maskz_loadu_epi8()
1780                  (__mmask64) __U);  in _mm512_maskz_loadu_epi8()
1810 _mm512_mask_storeu_epi8 (void *__P, __mmask64 __U, __m512i __A)  in _mm512_mask_storeu_epi8()
1814              (__mmask64) __U);  in _mm512_mask_storeu_epi8()
1817 static __inline__ __mmask64 __DEFAULT_FN_ATTRS512
1824 static __inline__ __mmask64 __DEFAULT_FN_ATTRS512
1825 _mm512_mask_test_epi8_mask (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_test_epi8_mask()
1845 static __inline__ __mmask64 __DEFAULT_FN_ATTRS512
1851 static __inline__ __mmask64 __DEFAULT_FN_ATTRS512
1852 _mm512_mask_testn_epi8_mask (__mmask64 __U, __m512i __A, __m512i __B)  in _mm512_mask_testn_epi8_mask()
1872 static __inline__ __mmask64 __DEFAULT_FN_ATTRS512
1875   return (__mmask64) __builtin_ia32_cvtb2mask512 ((__v64qi) __A);  in _mm512_movepi8_mask()
1885 _mm512_movm_epi8 (__mmask64 __A)  in _mm512_movm_epi8()
1907 _mm512_mask_broadcastb_epi8 (__m512i __O, __mmask64 __M, __m128i __A)  in _mm512_mask_broadcastb_epi8()
1915 _mm512_maskz_broadcastb_epi8 (__mmask64 __M, __m128i __A)  in _mm512_maskz_broadcastb_epi8()
1991   (__m512i)__builtin_ia32_selectb_512((__mmask64)(U), \
1996   (__m512i)__builtin_ia32_selectb_512((__mmask64)(U), \