diff options
| -rw-r--r-- | clang/lib/Headers/avx512fintrin.h | 34 | ||||
| -rw-r--r-- | clang/test/CodeGen/avx512f-builtins.c | 27 |
2 files changed, 61 insertions, 0 deletions
diff --git a/clang/lib/Headers/avx512fintrin.h b/clang/lib/Headers/avx512fintrin.h index 56f67ad1b8e..15cfd886e3b 100644 --- a/clang/lib/Headers/avx512fintrin.h +++ b/clang/lib/Headers/avx512fintrin.h @@ -1631,6 +1631,23 @@ _mm512_abs_epi64(__m512i __A) (__mmask8) -1); } +static __inline__ __m512i __DEFAULT_FN_ATTRS +_mm512_mask_abs_epi64 (__m512i __W, __mmask8 __U, __m512i __A) +{ + return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A, + (__v8di) __W, + (__mmask8) __U); +} + +static __inline__ __m512i __DEFAULT_FN_ATTRS +_mm512_maskz_abs_epi64 (__mmask8 __U, __m512i __A) +{ + return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A, + (__v8di) + _mm512_setzero_si512 (), + (__mmask8) __U); +} + static __inline __m512i __DEFAULT_FN_ATTRS _mm512_abs_epi32(__m512i __A) { @@ -1640,6 +1657,23 @@ _mm512_abs_epi32(__m512i __A) (__mmask16) -1); } +static __inline__ __m512i __DEFAULT_FN_ATTRS +_mm512_mask_abs_epi32 (__m512i __W, __mmask16 __U, __m512i __A) +{ + return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A, + (__v16si) __W, + (__mmask16) __U); +} + +static __inline__ __m512i __DEFAULT_FN_ATTRS +_mm512_maskz_abs_epi32 (__mmask16 __U, __m512i __A) +{ + return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A, + (__v16si) + _mm512_setzero_si512 (), + (__mmask16) __U); +} + static __inline__ __m128 __DEFAULT_FN_ATTRS _mm_mask_add_ss(__m128 __W, __mmask8 __U,__m128 __A, __m128 __B) { return (__m128) __builtin_ia32_addss_round_mask ((__v4sf) __A, diff --git a/clang/test/CodeGen/avx512f-builtins.c b/clang/test/CodeGen/avx512f-builtins.c index 7eae57c5d2b..d561ed0b813 100644 --- a/clang/test/CodeGen/avx512f-builtins.c +++ b/clang/test/CodeGen/avx512f-builtins.c @@ -6574,3 +6574,30 @@ __m512 test_mm512_set_ps (float __A, float __B, float __C, float __D, __I, __J, __K, __L, __M, __N, __O, __P); } +__m512i test_mm512_mask_abs_epi64 (__m512i __W, __mmask8 __U, __m512i __A) +{ + // CHECK-LABEL: @test_mm512_mask_abs_epi64 + // CHECK: @llvm.x86.avx512.mask.pabs.q.512 + return _mm512_mask_abs_epi64 (__W,__U,__A); +} + +__m512i test_mm512_maskz_abs_epi64 (__mmask8 __U, __m512i __A) +{ + // CHECK-LABEL: @test_mm512_maskz_abs_epi64 + // CHECK: @llvm.x86.avx512.mask.pabs.q.512 + return _mm512_maskz_abs_epi64 (__U,__A); +} + +__m512i test_mm512_mask_abs_epi32 (__m512i __W, __mmask16 __U, __m512i __A) +{ + // CHECK-LABEL: @test_mm512_mask_abs_epi32 + // CHECK: @llvm.x86.avx512.mask.pabs.d.512 + return _mm512_mask_abs_epi32 (__W,__U,__A); +} + +__m512i test_mm512_maskz_abs_epi32 (__mmask16 __U, __m512i __A) +{ + // CHECK-LABEL: @test_mm512_maskz_abs_epi32 + // CHECK: @llvm.x86.avx512.mask.pabs.d.512 + return _mm512_maskz_abs_epi32 (__U,__A); +} |
