diff options
| -rw-r--r-- | clang/lib/Headers/avx512fintrin.h | 84 | ||||
| -rw-r--r-- | clang/test/CodeGen/avx512f-builtins.c | 58 |
2 files changed, 142 insertions, 0 deletions
diff --git a/clang/lib/Headers/avx512fintrin.h b/clang/lib/Headers/avx512fintrin.h index b6188831e77..5a09b0141d9 100644 --- a/clang/lib/Headers/avx512fintrin.h +++ b/clang/lib/Headers/avx512fintrin.h @@ -735,6 +735,27 @@ _mm512_max_pd(__m512d __A, __m512d __B) _MM_FROUND_CUR_DIRECTION); } +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_mask_max_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) +{ + return (__m512d) __builtin_ia32_maxpd512_mask ((__v8df) __A, + (__v8df) __B, + (__v8df) __W, + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_maskz_max_pd (__mmask8 __U, __m512d __A, __m512d __B) +{ + return (__m512d) __builtin_ia32_maxpd512_mask ((__v8df) __A, + (__v8df) __B, + (__v8df) + _mm512_setzero_pd (), + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + static __inline__ __m512 __DEFAULT_FN_ATTRS _mm512_max_ps(__m512 __A, __m512 __B) { @@ -746,6 +767,27 @@ _mm512_max_ps(__m512 __A, __m512 __B) _MM_FROUND_CUR_DIRECTION); } +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_mask_max_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B) +{ + return (__m512) __builtin_ia32_maxps512_mask ((__v16sf) __A, + (__v16sf) __B, + (__v16sf) __W, + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_maskz_max_ps (__mmask16 __U, __m512 __A, __m512 __B) +{ + return (__m512) __builtin_ia32_maxps512_mask ((__v16sf) __A, + (__v16sf) __B, + (__v16sf) + _mm512_setzero_ps (), + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + static __inline__ __m128 __DEFAULT_FN_ATTRS _mm_mask_max_ss(__m128 __W, __mmask8 __U,__m128 __A, __m128 __B) { return (__m128) __builtin_ia32_maxss_round_mask ((__v4sf) __A, @@ -858,6 +900,27 @@ _mm512_min_pd(__m512d __A, __m512d __B) _MM_FROUND_CUR_DIRECTION); } +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_mask_min_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) +{ + return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A, + (__v8df) __B, + (__v8df) __W, + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_maskz_min_pd (__mmask8 __U, __m512d __A, __m512d __B) +{ + return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A, + (__v8df) __B, + (__v8df) + _mm512_setzero_pd (), + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + static __inline__ __m512 __DEFAULT_FN_ATTRS _mm512_min_ps(__m512 __A, __m512 __B) { @@ -869,6 +932,27 @@ _mm512_min_ps(__m512 __A, __m512 __B) _MM_FROUND_CUR_DIRECTION); } +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_mask_min_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B) +{ + return (__m512) __builtin_ia32_minps512_mask ((__v16sf) __A, + (__v16sf) __B, + (__v16sf) __W, + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_maskz_min_ps (__mmask16 __U, __m512 __A, __m512 __B) +{ + return (__m512) __builtin_ia32_minps512_mask ((__v16sf) __A, + (__v16sf) __B, + (__v16sf) + _mm512_setzero_ps (), + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + static __inline__ __m128 __DEFAULT_FN_ATTRS _mm_mask_min_ss(__m128 __W, __mmask8 __U,__m128 __A, __m128 __B) { return (__m128) __builtin_ia32_minss_round_mask ((__v4sf) __A, diff --git a/clang/test/CodeGen/avx512f-builtins.c b/clang/test/CodeGen/avx512f-builtins.c index bb463715dc8..7d88c2a6822 100644 --- a/clang/test/CodeGen/avx512f-builtins.c +++ b/clang/test/CodeGen/avx512f-builtins.c @@ -5966,3 +5966,61 @@ __m512i test_mm512_mask_cvtps_epu32 (__m512i __W, __mmask16 __U, __m512 __A) return _mm512_mask_cvtps_epu32( __W, __U, __A); } + +__m512d test_mm512_mask_max_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) +{ + // CHECK-LABEL: @test_mm512_mask_max_pd + // CHECK: @llvm.x86.avx512.mask.max.pd.512 + return _mm512_mask_max_pd (__W,__U,__A,__B); +} + +__m512d test_mm512_maskz_max_pd (__mmask8 __U, __m512d __A, __m512d __B) +{ + // CHECK-LABEL: @test_mm512_maskz_max_pd + // CHECK: @llvm.x86.avx512.mask.max.pd.512 + return _mm512_maskz_max_pd (__U,__A,__B); +} + +__m512 test_mm512_mask_max_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B) +{ + // CHECK-LABEL: @test_mm512_mask_max_ps + // CHECK: @llvm.x86.avx512.mask.max.ps.512 + return _mm512_mask_max_ps (__W,__U,__A,__B); +} + +__m512 test_mm512_maskz_max_ps (__mmask16 __U, __m512 __A, __m512 __B) +{ + // CHECK-LABEL: @test_mm512_maskz_max_ps + // CHECK: @llvm.x86.avx512.mask.max.ps.512 + return _mm512_maskz_max_ps (__U,__A,__B); +} + +__m512d test_mm512_mask_min_pd (__m512d __W, __mmask8 __U, __m512d __A, __m512d __B) +{ + // CHECK-LABEL: @test_mm512_mask_min_pd + // CHECK: @llvm.x86.avx512.mask.min.pd.512 + return _mm512_mask_min_pd (__W,__U,__A,__B); +} + +__m512d test_mm512_maskz_min_pd (__mmask8 __U, __m512d __A, __m512d __B) +{ + // CHECK-LABEL: @test_mm512_maskz_min_pd + // CHECK: @llvm.x86.avx512.mask.min.pd.512 + return _mm512_maskz_min_pd (__U,__A,__B); +} + +__m512 test_mm512_mask_min_ps (__m512 __W, __mmask16 __U, __m512 __A, __m512 __B) +{ + // CHECK-LABEL: @test_mm512_mask_min_ps + // CHECK: @llvm.x86.avx512.mask.min.ps.512 + return _mm512_mask_min_ps (__W,__U,__A,__B); +} + +__m512 test_mm512_maskz_min_ps (__mmask16 __U, __m512 __A, __m512 __B) +{ + // CHECK-LABEL: @test_mm512_maskz_min_ps + // CHECK: @llvm.x86.avx512.mask.min.ps.512 + return _mm512_maskz_min_ps (__U,__A,__B); +} + + |
