forked from OSchip/llvm-project
[X86] Replace the mask cmpeq/cmple/cmplt/cmpgt/cmpge/cmpneq intrinsics with macros that just pass the right comparison predicate value to the regular cmp intrinsic. Remove mask cmpeq/cmpgt builtins that are now unused.
This shortens the intrinsic headers a little and allows us to get rid of the cmpeq and cmpgt handling from CGBuiltin.cpp. llvm-svn: 317506
This commit is contained in:
Craig Topper
parent
6bde1667ba
commit
57f96ac6dc
|
|
@ -910,39 +910,10 @@ TARGET_BUILTIN(__builtin_ia32_cvttps2dq512_mask, "V16iV16fV16iUsIi", "", "avx512
|
|||
TARGET_BUILTIN(__builtin_ia32_cvttps2udq512_mask, "V16iV16fV16iUsIi", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_cvttpd2dq512_mask, "V8iV8dV8iUcIi", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_cvttpd2udq512_mask, "V8iV8dV8iUcIi", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_cmpps512_mask, "UsV16fV16fIiUsIi", "", "avx512f")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_cmpps512_mask, "UsV16fV16fIiUsIi", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_cmpps256_mask, "UcV8fV8fIiUc", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_cmpps128_mask, "UcV4fV4fIiUc", "", "avx512vl")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqb512_mask, "LLiV64cV64cLLi", "", "avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqd512_mask, "sV16iV16is", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqq512_mask, "cV8LLiV8LLic", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqw512_mask, "iV32sV32si", "", "avx512bw")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqb256_mask, "iV32cV32ci", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqd256_mask, "cV8iV8ic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqq256_mask, "cV4LLiV4LLic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqw256_mask, "sV16sV16ss", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqb128_mask, "sV16cV16cs", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqd128_mask, "cV4iV4ic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqq128_mask, "cV2LLiV2LLic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpeqw128_mask, "cV8sV8sc", "", "avx512vl,avx512bw")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtb512_mask, "LLiV64cV64cLLi", "", "avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtd512_mask, "sV16iV16is", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtq512_mask, "cV8LLiV8LLic", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtw512_mask, "iV32sV32si", "", "avx512bw")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtb256_mask, "iV32cV32ci", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtd256_mask, "cV8iV8ic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtq256_mask, "cV4LLiV4LLic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtw256_mask, "sV16sV16ss", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtb128_mask, "sV16cV16cs", "", "avx512vl,avx512bw")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtd128_mask, "cV4iV4ic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtq128_mask, "cV2LLiV2LLic", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_pcmpgtw128_mask, "cV8sV8sc", "", "avx512vl,avx512bw")
|
||||
|
||||
TARGET_BUILTIN(__builtin_ia32_cmppd512_mask, "UcV8dV8dIiUcIi", "", "avx512f")
|
||||
TARGET_BUILTIN(__builtin_ia32_cmppd256_mask, "UcV4dV4dIiUc", "", "avx512vl")
|
||||
TARGET_BUILTIN(__builtin_ia32_cmppd128_mask, "UcV2dV2dIiUc", "", "avx512vl")
|
||||
|
|
|
|||
|
|
@ -8142,32 +8142,6 @@ Value *CodeGenFunction::EmitX86BuiltinExpr(unsigned BuiltinID,
|
|||
case X86::BI__builtin_ia32_selectpd_256:
|
||||
case X86::BI__builtin_ia32_selectpd_512:
|
||||
return EmitX86Select(*this, Ops[0], Ops[1], Ops[2]);
|
||||
case X86::BI__builtin_ia32_pcmpeqb128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqb256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqb512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqw128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqw256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqw512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqd128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqd256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqd512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqq128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqq256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpeqq512_mask:
|
||||
return EmitX86MaskedCompare(*this, 0, false, Ops);
|
||||
case X86::BI__builtin_ia32_pcmpgtb128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtb256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtb512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtw128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtw256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtw512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtd128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtd256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtd512_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtq128_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtq256_mask:
|
||||
case X86::BI__builtin_ia32_pcmpgtq512_mask:
|
||||
return EmitX86MaskedCompare(*this, 6, true, Ops);
|
||||
case X86::BI__builtin_ia32_cmpb128_mask:
|
||||
case X86::BI__builtin_ia32_cmpb256_mask:
|
||||
case X86::BI__builtin_ia32_cmpb512_mask:
|
||||
|
|
|
|||
|
|
@ -56,293 +56,145 @@ _mm512_setzero_hi(void) {
|
|||
|
||||
/* Integer compare */
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_pcmpeqb512_mask((__v64qi)__a, (__v64qi)__b,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
#define _mm512_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)-1); })
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_pcmpeqb512_mask((__v64qi)__a, (__v64qi)__b,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)(m)); })
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 0,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
#define _mm512_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)-1); })
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)(m)); })
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpeqw512_mask((__v32hi)__a, (__v32hi)__b,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
#define _mm512_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpeqw512_mask((__v32hi)__a, (__v32hi)__b,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 0,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
#define _mm512_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
#define _mm512_cmpeq_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epi8_mask(A, B) \
|
||||
_mm512_cmp_epi8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epi8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_cmpeq_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epu8_mask(A, B) \
|
||||
_mm512_cmp_epu8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epu8_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
#define _mm512_cmpeq_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epi16_mask(A, B) \
|
||||
_mm512_cmp_epi16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epi16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 5,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 5,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_pcmpgtb512_mask((__v64qi)__a, (__v64qi)__b,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_pcmpgtb512_mask((__v64qi)__a, (__v64qi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 6,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpgtw512_mask((__v32hi)__a, (__v32hi)__b,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpgtw512_mask((__v32hi)__a, (__v32hi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 6,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 2,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 2,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 1,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 1,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epi8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epi8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epu8_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,
|
||||
(__mmask64)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epu8_mask(__mmask64 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)__a, (__v64qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epi16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 4,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epi16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)__a, (__v32hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epu16_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 4,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epu16_mask(__mmask32 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)__a, (__v32hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_cmpeq_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epu16_mask(A, B) \
|
||||
_mm512_cmp_epu16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epu16_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __m512i __DEFAULT_FN_ATTRS
|
||||
_mm512_add_epi8 (__m512i __A, __m512i __B) {
|
||||
|
|
@ -1541,46 +1393,6 @@ _mm512_maskz_cvtepu8_epi16(__mmask32 __U, __m256i __A)
|
|||
}
|
||||
|
||||
|
||||
#define _mm512_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)-1); })
|
||||
|
||||
#define _mm512_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_cmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)(m)); })
|
||||
|
||||
#define _mm512_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)-1); })
|
||||
|
||||
#define _mm512_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask64)__builtin_ia32_ucmpb512_mask((__v64qi)(__m512i)(a), \
|
||||
(__v64qi)(__m512i)(b), (int)(p), \
|
||||
(__mmask64)(m)); })
|
||||
|
||||
#define _mm512_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm512_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm512_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm512_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpw512_mask((__v32hi)(__m512i)(a), \
|
||||
(__v32hi)(__m512i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm512_shufflehi_epi16(A, imm) __extension__ ({ \
|
||||
(__m512i)__builtin_shufflevector((__v32hi)(__m512i)(A), \
|
||||
(__v32hi)_mm512_undefined_epi32(), \
|
||||
|
|
|
|||
|
|
@ -4844,293 +4844,105 @@ _mm512_knot(__mmask16 __M)
|
|||
|
||||
/* Integer compare */
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqd512_mask((__v16si)__a, (__v16si)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
#define _mm512_cmpeq_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epi32_mask(A, B) \
|
||||
_mm512_cmp_epi32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epi32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqd512_mask((__v16si)__a, (__v16si)__b,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_cmpeq_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epu32_mask(A, B) \
|
||||
_mm512_cmp_epu32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epu32_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 0,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
#define _mm512_cmpeq_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epi64_mask(A, B) \
|
||||
_mm512_cmp_epi64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epi64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq512_mask((__v8di)__a, (__v8di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq512_mask((__v8di)__a, (__v8di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpeq_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpeq_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpge_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpge_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtd512_mask((__v16si)__a, (__v16si)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtd512_mask((__v16si)__a, (__v16si)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 6,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq512_mask((__v8di)__a, (__v8di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq512_mask((__v8di)__a, (__v8di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpgt_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpgt_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmple_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmple_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmplt_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmplt_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epi32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epi32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpd512_mask((__v16si)__a, (__v16si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epu32_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpd512_mask((__v16si)__a, (__v16si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epi64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epi64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq512_mask((__v8di)__a, (__v8di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_cmpneq_epu64_mask(__m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm512_mask_cmpneq_epu64_mask(__mmask8 __u, __m512i __a, __m512i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq512_mask((__v8di)__a, (__v8di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
#define _mm512_cmpeq_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_mask_cmpeq_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm512_cmpge_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_mask_cmpge_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm512_cmpgt_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_mask_cmpgt_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm512_cmple_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_mask_cmple_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm512_cmplt_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_mask_cmplt_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm512_cmpneq_epu64_mask(A, B) \
|
||||
_mm512_cmp_epu64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm512_mask_cmpneq_epu64_mask(k, A, B) \
|
||||
_mm512_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __m512i __DEFAULT_FN_ATTRS
|
||||
_mm512_cvtepi8_epi32(__m128i __A)
|
||||
|
|
|
|||
|
|
@ -38,581 +38,285 @@ _mm_setzero_hi(void){
|
|||
|
||||
/* Integer compare */
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqb128_mask((__v16qi)__a, (__v16qi)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqb128_mask((__v16qi)__a, (__v16qi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 0,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpeqb256_mask((__v32qi)__a, (__v32qi)__b,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpeqb256_mask((__v32qi)__a, (__v32qi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 0,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqw128_mask((__v8hi)__a, (__v8hi)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqw128_mask((__v8hi)__a, (__v8hi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqw256_mask((__v16hi)__a, (__v16hi)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpeqw256_mask((__v16hi)__a, (__v16hi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 0,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 5,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtb128_mask((__v16qi)__a, (__v16qi)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtb128_mask((__v16qi)__a, (__v16qi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 6,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpgtb256_mask((__v32qi)__a, (__v32qi)__b,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_pcmpgtb256_mask((__v32qi)__a, (__v32qi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 6,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtw128_mask((__v8hi)__a, (__v8hi)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtw128_mask((__v8hi)__a, (__v8hi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtw256_mask((__v16hi)__a, (__v16hi)__b,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_pcmpgtw256_mask((__v16hi)__a, (__v16hi)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 6,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 2,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 1,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epi8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epi8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)__a, (__v16qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epu8_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epu8_mask(__mmask16 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)__a, (__v16qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epi8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epi8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epu8_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,
|
||||
(__mmask32)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask32 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epu8_mask(__mmask32 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)__a, (__v32qi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epi16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epi16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)__a, (__v8hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epu16_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epu16_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)__a, (__v8hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epi16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epi16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)__a, (__v16hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epu16_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 4,
|
||||
(__mmask16)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask16 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epu16_mask(__mmask16 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)__a, (__v16hi)__b, 4,
|
||||
__u);
|
||||
}
|
||||
#define _mm_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm256_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm256_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)(m)); })
|
||||
|
||||
#define _mm_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)(m)); })
|
||||
|
||||
#define _mm256_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm256_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm_cmpeq_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epi8_mask(A, B) \
|
||||
_mm_cmp_epi8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epi8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epi8_mask(A, B) \
|
||||
_mm256_cmp_epi8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epi8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epu8_mask(A, B) \
|
||||
_mm_cmp_epu8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epu8_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epu8_mask(A, B) \
|
||||
_mm256_cmp_epu8_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epu8_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu8_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epi16_mask(A, B) \
|
||||
_mm_cmp_epi16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epi16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epi16_mask(A, B) \
|
||||
_mm256_cmp_epi16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epi16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epu16_mask(A, B) \
|
||||
_mm_cmp_epu16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epu16_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epu16_mask(A, B) \
|
||||
_mm256_cmp_epu16_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epu16_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu16_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __m256i __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_add_epi8(__m256i __W, __mmask32 __U, __m256i __A, __m256i __B){
|
||||
|
|
@ -2146,86 +1850,6 @@ _mm256_maskz_cvtepu8_epi16 (__mmask16 __U, __m128i __A)
|
|||
}
|
||||
|
||||
|
||||
#define _mm_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpb128_mask((__v16qi)(__m128i)(a), \
|
||||
(__v16qi)(__m128i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm256_cmp_epi8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epi8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_cmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm256_cmp_epu8_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epu8_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask32)__builtin_ia32_ucmpb256_mask((__v32qi)(__m256i)(a), \
|
||||
(__v32qi)(__m256i)(b), (int)(p), \
|
||||
(__mmask32)(m)); })
|
||||
|
||||
#define _mm_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_cmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)(m)); })
|
||||
|
||||
#define _mm_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)-1); })
|
||||
|
||||
#define _mm_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask8)__builtin_ia32_ucmpw128_mask((__v8hi)(__m128i)(a), \
|
||||
(__v8hi)(__m128i)(b), (int)(p), \
|
||||
(__mmask8)(m)); })
|
||||
|
||||
#define _mm256_cmp_epi16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epi16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_cmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm256_cmp_epu16_mask(a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)-1); })
|
||||
|
||||
#define _mm256_mask_cmp_epu16_mask(m, a, b, p) __extension__ ({ \
|
||||
(__mmask16)__builtin_ia32_ucmpw256_mask((__v16hi)(__m256i)(a), \
|
||||
(__v16hi)(__m256i)(b), (int)(p), \
|
||||
(__mmask16)(m)); })
|
||||
|
||||
#define _mm_mask_shufflehi_epi16(W, U, A, imm) __extension__ ({ \
|
||||
(__m128i)__builtin_ia32_selectw_128((__mmask8)(U), \
|
||||
(__v8hi)_mm_shufflehi_epi16((A), (imm)), \
|
||||
|
|
|
|||
|
|
@ -38,582 +38,205 @@ _mm_setzero_di(void) {
|
|||
|
||||
/* Integer compare */
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqd128_mask((__v4si)__a, (__v4si)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqd128_mask((__v4si)__a, (__v4si)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqd256_mask((__v8si)__a, (__v8si)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqd256_mask((__v8si)__a, (__v8si)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq128_mask((__v2di)__a, (__v2di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq128_mask((__v2di)__a, (__v2di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpeq_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpeq_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq256_mask((__v4di)__a, (__v4di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpeqq256_mask((__v4di)__a, (__v4di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpeq_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 0,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpeq_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 0,
|
||||
__u);
|
||||
}
|
||||
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpge_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpge_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpge_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 5,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpge_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 5,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtd128_mask((__v4si)__a, (__v4si)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtd128_mask((__v4si)__a, (__v4si)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtd256_mask((__v8si)__a, (__v8si)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtd256_mask((__v8si)__a, (__v8si)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq128_mask((__v2di)__a, (__v2di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq128_mask((__v2di)__a, (__v2di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpgt_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpgt_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq256_mask((__v4di)__a, (__v4di)__b,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_pcmpgtq256_mask((__v4di)__a, (__v4di)__b,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpgt_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 6,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpgt_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 6,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmple_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmple_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmple_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 2,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmple_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 2,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmplt_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmplt_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmplt_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 1,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmplt_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 1,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epi32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd128_mask((__v4si)__a, (__v4si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epu32_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epu32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd128_mask((__v4si)__a, (__v4si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epi32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpd256_mask((__v8si)__a, (__v8si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epu32_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epu32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpd256_mask((__v8si)__a, (__v8si)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epi64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq128_mask((__v2di)__a, (__v2di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_cmpneq_epu64_mask(__m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm_mask_cmpneq_epu64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq128_mask((__v2di)__a, (__v2di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epi64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_cmpq256_mask((__v4di)__a, (__v4di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_cmpneq_epu64_mask(__m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 4,
|
||||
(__mmask8)-1);
|
||||
}
|
||||
|
||||
static __inline__ __mmask8 __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_cmpneq_epu64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
|
||||
return (__mmask8)__builtin_ia32_ucmpq256_mask((__v4di)__a, (__v4di)__b, 4,
|
||||
__u);
|
||||
}
|
||||
#define _mm_cmpeq_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epi32_mask(A, B) \
|
||||
_mm_cmp_epi32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epi32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epi32_mask(A, B) \
|
||||
_mm256_cmp_epi32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epi32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epu32_mask(A, B) \
|
||||
_mm_cmp_epu32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epu32_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epu32_mask(A, B) \
|
||||
_mm256_cmp_epu32_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epu32_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu32_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epi64_mask(A, B) \
|
||||
_mm_cmp_epi64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epi64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epi64_mask(A, B) \
|
||||
_mm256_cmp_epi64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epi64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epi64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm_cmpeq_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_mask_cmpeq_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm_cmpge_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_mask_cmpge_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm_cmpgt_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_mask_cmpgt_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm_cmple_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_mask_cmple_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm_cmplt_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_mask_cmplt_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm_cmpneq_epu64_mask(A, B) \
|
||||
_mm_cmp_epu64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm_mask_cmpneq_epu64_mask(k, A, B) \
|
||||
_mm_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
#define _mm256_cmpeq_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_mask_cmpeq_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_EQ)
|
||||
#define _mm256_cmpge_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_mask_cmpge_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GE)
|
||||
#define _mm256_cmpgt_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_mask_cmpgt_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_GT)
|
||||
#define _mm256_cmple_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_mask_cmple_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LE)
|
||||
#define _mm256_cmplt_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_mask_cmplt_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_LT)
|
||||
#define _mm256_cmpneq_epu64_mask(A, B) \
|
||||
_mm256_cmp_epu64_mask((A), (B), _MM_CMPINT_NE)
|
||||
#define _mm256_mask_cmpneq_epu64_mask(k, A, B) \
|
||||
_mm256_mask_cmp_epu64_mask((k), (A), (B), _MM_CMPINT_NE)
|
||||
|
||||
static __inline__ __m256i __DEFAULT_FN_ATTRS
|
||||
_mm256_mask_add_epi32(__m256i __W, __mmask8 __U, __m256i __A, __m256i __B)
|
||||
|
|
|
|||
Loading…
Reference in New Issue