32 typedef unsigned long long __mmask64;  typedef
39 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
41   return (__mmask64)__builtin_ia32_pcmpeqb512_mask((__v64qi)__a, (__v64qi)__b,  in _mm512_cmpeq_epi8_mask()
42                                                    (__mmask64)-1);  in _mm512_cmpeq_epi8_mask()
45 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
46 _mm512_mask_cmpeq_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpeq_epi8_mask()
47   return (__mmask64)__builtin_ia32_pcmpeqb512_mask((__v64qi)__a, (__v64qi)__b,  in _mm512_mask_cmpeq_epi8_mask()
51 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
53   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 0,  in _mm512_cmpeq_epu8_mask()
54                                                  (__mmask64)-1);  in _mm512_cmpeq_epu8_mask()
57 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
58 _mm512_mask_cmpeq_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpeq_epu8_mask()
59   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 0,  in _mm512_mask_cmpeq_epu8_mask()
87 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
89   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,  in _mm512_cmpge_epi8_mask()
90                                                 (__mmask64)-1);  in _mm512_cmpge_epi8_mask()
93 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
94 _mm512_mask_cmpge_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpge_epi8_mask()
95   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,  in _mm512_mask_cmpge_epi8_mask()
99 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
101   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,  in _mm512_cmpge_epu8_mask()
102                                                  (__mmask64)-1);  in _mm512_cmpge_epu8_mask()
105 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
106 _mm512_mask_cmpge_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpge_epu8_mask()
107   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,  in _mm512_mask_cmpge_epu8_mask()
135 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
137   return (__mmask64)__builtin_ia32_pcmpgtb512_mask((__v64qi)__a, (__v64qi)__b,  in _mm512_cmpgt_epi8_mask()
138                                                    (__mmask64)-1);  in _mm512_cmpgt_epi8_mask()
141 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
142 _mm512_mask_cmpgt_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpgt_epi8_mask()
143   return (__mmask64)__builtin_ia32_pcmpgtb512_mask((__v64qi)__a, (__v64qi)__b,  in _mm512_mask_cmpgt_epi8_mask()
147 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
149   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 6,  in _mm512_cmpgt_epu8_mask()
150                                                  (__mmask64)-1);  in _mm512_cmpgt_epu8_mask()
153 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
154 _mm512_mask_cmpgt_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpgt_epu8_mask()
155   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 6,  in _mm512_mask_cmpgt_epu8_mask()
183 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
185   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,  in _mm512_cmple_epi8_mask()
186                                                 (__mmask64)-1);  in _mm512_cmple_epi8_mask()
189 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
190 _mm512_mask_cmple_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmple_epi8_mask()
191   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,  in _mm512_mask_cmple_epi8_mask()
195 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
197   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,  in _mm512_cmple_epu8_mask()
198                                                  (__mmask64)-1);  in _mm512_cmple_epu8_mask()
201 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
202 _mm512_mask_cmple_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmple_epu8_mask()
203   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,  in _mm512_mask_cmple_epu8_mask()
231 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
233   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,  in _mm512_cmplt_epi8_mask()
234                                                 (__mmask64)-1);  in _mm512_cmplt_epi8_mask()
237 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
238 _mm512_mask_cmplt_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmplt_epi8_mask()
239   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,  in _mm512_mask_cmplt_epi8_mask()
243 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
245   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,  in _mm512_cmplt_epu8_mask()
246                                                  (__mmask64)-1);  in _mm512_cmplt_epu8_mask()
249 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
250 _mm512_mask_cmplt_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmplt_epu8_mask()
251   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,  in _mm512_mask_cmplt_epu8_mask()
279 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
281   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,  in _mm512_cmpneq_epi8_mask()
282                                                 (__mmask64)-1);  in _mm512_cmpneq_epi8_mask()
285 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
286 _mm512_mask_cmpneq_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpneq_epi8_mask()
287   return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,  in _mm512_mask_cmpneq_epi8_mask()
291 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
293   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,  in _mm512_cmpneq_epu8_mask()
294                                                  (__mmask64)-1);  in _mm512_cmpneq_epu8_mask()
297 static __inline__ __mmask64 __attribute__((__always_inline__, __nodebug__))
298 _mm512_mask_cmpneq_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {  in _mm512_mask_cmpneq_epu8_mask()
299   return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,  in _mm512_mask_cmpneq_epu8_mask()
330                                          (p), (__mmask64)-1); })
335                                          (p), (__mmask64)(m)); })
340                                           (p), (__mmask64)-1); })
345                                           (p), (__mmask64)(m)); })