57 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
59   return (__mmask32)__builtin_ia32_pcmpeqb256_mask((__v32qi)__a, (__v32qi)__b,  in _mm256_cmpeq_epi8_mask()
60                                                    (__mmask32)-1);  in _mm256_cmpeq_epi8_mask()
63 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
64 _mm256_mask_cmpeq_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpeq_epi8_mask()
65   return (__mmask32)__builtin_ia32_pcmpeqb256_mask((__v32qi)__a, (__v32qi)__b,  in _mm256_mask_cmpeq_epi8_mask()
69 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
71   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 0,  in _mm256_cmpeq_epu8_mask()
72                                                  (__mmask32)-1);  in _mm256_cmpeq_epu8_mask()
75 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
76 _mm256_mask_cmpeq_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpeq_epu8_mask()
77   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 0,  in _mm256_mask_cmpeq_epu8_mask()
153 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
155   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,  in _mm256_cmpge_epi8_mask()
156                                                 (__mmask32)-1);  in _mm256_cmpge_epi8_mask()
159 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
160 _mm256_mask_cmpge_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpge_epi8_mask()
161   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,  in _mm256_mask_cmpge_epi8_mask()
165 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
167   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,  in _mm256_cmpge_epu8_mask()
168                                                  (__mmask32)-1);  in _mm256_cmpge_epu8_mask()
171 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
172 _mm256_mask_cmpge_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpge_epu8_mask()
173   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,  in _mm256_mask_cmpge_epu8_mask()
249 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
251   return (__mmask32)__builtin_ia32_pcmpgtb256_mask((__v32qi)__a, (__v32qi)__b,  in _mm256_cmpgt_epi8_mask()
252                                                    (__mmask32)-1);  in _mm256_cmpgt_epi8_mask()
255 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
256 _mm256_mask_cmpgt_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpgt_epi8_mask()
257   return (__mmask32)__builtin_ia32_pcmpgtb256_mask((__v32qi)__a, (__v32qi)__b,  in _mm256_mask_cmpgt_epi8_mask()
261 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
263   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 6,  in _mm256_cmpgt_epu8_mask()
264                                                  (__mmask32)-1);  in _mm256_cmpgt_epu8_mask()
267 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
268 _mm256_mask_cmpgt_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpgt_epu8_mask()
269   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 6,  in _mm256_mask_cmpgt_epu8_mask()
345 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
347   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,  in _mm256_cmple_epi8_mask()
348                                                 (__mmask32)-1);  in _mm256_cmple_epi8_mask()
351 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
352 _mm256_mask_cmple_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmple_epi8_mask()
353   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,  in _mm256_mask_cmple_epi8_mask()
357 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
359   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,  in _mm256_cmple_epu8_mask()
360                                                  (__mmask32)-1);  in _mm256_cmple_epu8_mask()
363 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
364 _mm256_mask_cmple_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmple_epu8_mask()
365   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,  in _mm256_mask_cmple_epu8_mask()
441 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
443   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,  in _mm256_cmplt_epi8_mask()
444                                                 (__mmask32)-1);  in _mm256_cmplt_epi8_mask()
447 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
448 _mm256_mask_cmplt_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmplt_epi8_mask()
449   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,  in _mm256_mask_cmplt_epi8_mask()
453 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
455   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,  in _mm256_cmplt_epu8_mask()
456                                                  (__mmask32)-1);  in _mm256_cmplt_epu8_mask()
459 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
460 _mm256_mask_cmplt_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmplt_epu8_mask()
461   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,  in _mm256_mask_cmplt_epu8_mask()
537 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
539   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,  in _mm256_cmpneq_epi8_mask()
540                                                 (__mmask32)-1);  in _mm256_cmpneq_epi8_mask()
543 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
544 _mm256_mask_cmpneq_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpneq_epi8_mask()
545   return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,  in _mm256_mask_cmpneq_epi8_mask()
549 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
551   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,  in _mm256_cmpneq_epu8_mask()
552                                                  (__mmask32)-1);  in _mm256_cmpneq_epu8_mask()
555 static __inline__ __mmask32 __attribute__((__always_inline__, __nodebug__))
556 _mm256_mask_cmpneq_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {  in _mm256_mask_cmpneq_epu8_mask()
557   return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,  in _mm256_mask_cmpneq_epu8_mask()
630   (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
632                                          (p), (__mmask32)-1); })
635   (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
637                                          (p), (__mmask32)(m)); })
640   (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
642                                           (p), (__mmask32)-1); })
645   (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
647                                           (p), (__mmask32)(m)); })