diff --git a/clang/include/clang/Basic/BuiltinsX86.def b/clang/include/clang/Basic/BuiltinsX86.def index 0fd3bab2d577..c153f6692dcf 100644 --- a/clang/include/clang/Basic/BuiltinsX86.def +++ b/clang/include/clang/Basic/BuiltinsX86.def @@ -2121,6 +2121,14 @@ TARGET_BUILTIN(__builtin_ia32_insertf64x2_256_mask, "V4dV4dV2dIiV4dUc","","avx51 TARGET_BUILTIN(__builtin_ia32_inserti64x2_256_mask, "V4LLiV4LLiV2LLiIiV4LLiUc","","avx512dq,avx512vl") TARGET_BUILTIN(__builtin_ia32_insertf32x4_256_mask, "V8fV8fV4fIiV8fUc","","avx512vl") TARGET_BUILTIN(__builtin_ia32_inserti32x4_256_mask, "V8iV8iV4iIiV8iUc","","avx512vl") +TARGET_BUILTIN(__builtin_ia32_getmantpd128_mask, "V2dV2diV2dUc","","avx512vl") +TARGET_BUILTIN(__builtin_ia32_getmantpd256_mask, "V4dV4diV4dUc","","avx512vl") +TARGET_BUILTIN(__builtin_ia32_getmantps128_mask, "V4fV4fiV4fUc","","avx512vl") +TARGET_BUILTIN(__builtin_ia32_getmantps256_mask, "V8fV8fiV8fUc","","avx512vl") +TARGET_BUILTIN(__builtin_ia32_getmantpd512_mask, "V8dV8diV8dUcIi","","avx512f") +TARGET_BUILTIN(__builtin_ia32_getmantps512_mask, "V16fV16fiV16fUsIi","","avx512f") +TARGET_BUILTIN(__builtin_ia32_getexppd512_mask, "V8dV8dV8dUcIi","","avx512f") +TARGET_BUILTIN(__builtin_ia32_getexpps512_mask, "V16fV16fV16fUsIi","","avx512f") #undef BUILTIN #undef TARGET_BUILTIN diff --git a/clang/lib/Headers/avx512fintrin.h b/clang/lib/Headers/avx512fintrin.h index 19115b74f964..65e7851e2fed 100644 --- a/clang/lib/Headers/avx512fintrin.h +++ b/clang/lib/Headers/avx512fintrin.h @@ -6148,6 +6148,179 @@ __builtin_ia32_inserti64x4_mask ((__v8di)( __A),\ (__mmask8)( __U));\ }) +#define _mm512_getmant_round_pd( __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df) _mm512_undefined_pd (),\ + (__mmask8) -1,( __R));\ +}) + +#define _mm512_mask_getmant_round_pd( __W, __U, __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df)( __W),(__mmask8)( __U),\ + ( __R));\ +}) + +#define _mm512_maskz_getmant_round_pd( __U, __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df) _mm512_setzero_pd (),\ + (__mmask8)( __U),( __R));\ +}) + +#define _mm512_getmant_pd( __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df) _mm512_setzero_pd (),\ + (__mmask8) -1, _MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_mask_getmant_pd( __W, __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df)( __W), (__mmask8)( __U), _MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_maskz_getmant_pd( __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd512_mask ((__v8df)( __A),\ + (__C << 2) |( __B),\ + (__v8df) _mm512_setzero_pd (),\ + (__mmask8)( __U), _MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_getmant_round_ps( __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf) _mm512_undefined_ps (),\ + (__mmask16) -1,( __R));\ +}) + +#define _mm512_mask_getmant_round_ps( __W, __U, __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf)( __W),(__mmask16)( __U),\ + ( __R));\ +}) + +#define _mm512_maskz_getmant_round_ps( __U, __A, __B, __C, __R) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf) _mm512_setzero_ps (),\ + ( __U),( __R));\ +}) + +#define _mm512_getmant_ps( __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf) _mm512_undefined_ps (),\ + (__mmask16) -1, _MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_mask_getmant_ps( __W, __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf)( __W),(__mmask16) ( __U),\ + _MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_maskz_getmant_ps( __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps512_mask ((__v16sf)( __A),\ + (__C << 2) |( __B),\ + (__v16sf) _mm512_setzero_ps (),\ + (__mmask16)( __U),_MM_FROUND_CUR_DIRECTION);\ +}) + +#define _mm512_getexp_round_pd( __A, __R) __extension__ ({ \ +__builtin_ia32_getexppd512_mask ((__v8df)( __A),\ + (__v8df) _mm512_undefined_pd (),\ + (__mmask8) -1,( __R));\ +}) + +#define _mm512_mask_getexp_round_pd( __W, __U, __A, __R) __extension__ ({ \ +__builtin_ia32_getexppd512_mask ((__v8df)( __A),\ + (__v8df)( __W),\ + (__mmask8)( __U),( __R));\ +}) + +#define _mm512_maskz_getexp_round_pd( __U, __A, __R) __extension__ ({ \ +__builtin_ia32_getexppd512_mask ((__v8df)( __A),\ + (__v8df) _mm512_setzero_pd (),\ + (__mmask8)( __U),( __R));\ +}) + +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_getexp_pd (__m512d __A) +{ + return (__m512d) __builtin_ia32_getexppd512_mask ((__v8df) __A, + (__v8df) _mm512_undefined_pd (), + (__mmask8) -1, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_mask_getexp_pd (__m512d __W, __mmask8 __U, __m512d __A) +{ + return (__m512d) __builtin_ia32_getexppd512_mask ((__v8df) __A, + (__v8df) __W, + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512d __DEFAULT_FN_ATTRS +_mm512_maskz_getexp_pd (__mmask8 __U, __m512d __A) +{ + return (__m512d) __builtin_ia32_getexppd512_mask ((__v8df) __A, + (__v8df) _mm512_setzero_pd (), + (__mmask8) __U, + _MM_FROUND_CUR_DIRECTION); +} + +#define _mm512_getexp_round_ps( __A, __R) __extension__ ({ \ +__builtin_ia32_getexpps512_mask ((__v16sf)( __A),\ + (__v16sf) _mm512_undefined_ps (),\ + (__mmask16) -1,( __R));\ +}) + +#define _mm512_mask_getexp_round_ps( __W, __U, __A, __R) __extension__ ({ \ +__builtin_ia32_getexpps512_mask ((__v16sf)( __A),\ + (__v16sf)( __W),\ + (__mmask16)( __U),( __R));\ +}) + +#define _mm512_maskz_getexp_round_ps( __U, __A, __R) __extension__ ({ \ +__builtin_ia32_getexpps512_mask ((__v16sf)( __A),\ + (__v16sf) _mm512_setzero_ps (),\ + (__mmask16)( __U),( __R));\ +}) + +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_getexp_ps (__m512 __A) +{ + return (__m512) __builtin_ia32_getexpps512_mask ((__v16sf) __A, + (__v16sf) _mm512_undefined_ps (), + (__mmask16) -1, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_mask_getexp_ps (__m512 __W, __mmask16 __U, __m512 __A) +{ + return (__m512) __builtin_ia32_getexpps512_mask ((__v16sf) __A, + (__v16sf) __W, + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + +static __inline__ __m512 __DEFAULT_FN_ATTRS +_mm512_maskz_getexp_ps (__mmask16 __U, __m512 __A) +{ + return (__m512) __builtin_ia32_getexpps512_mask ((__v16sf) __A, + (__v16sf) _mm512_setzero_ps (), + (__mmask16) __U, + _MM_FROUND_CUR_DIRECTION); +} + #undef __DEFAULT_FN_ATTRS #endif // __AVX512FINTRIN_H diff --git a/clang/lib/Headers/avx512vlintrin.h b/clang/lib/Headers/avx512vlintrin.h index 8934f33373d6..78b79a02d480 100644 --- a/clang/lib/Headers/avx512vlintrin.h +++ b/clang/lib/Headers/avx512vlintrin.h @@ -8894,6 +8894,90 @@ __builtin_ia32_inserti32x4_256_mask ((__v8si)( __A),\ (__mmask8) ( __U));\ }) +#define _mm_getmant_pd( __A, __B, __C) __extension__({\ +__builtin_ia32_getmantpd128_mask ((__v2df) __A,\ + (__C << 2) | __B,\ + (__v2df) _mm_setzero_pd (),\ + (__mmask8) -1);\ +}) + +#define _mm_mask_getmant_pd( __W, __U, __A, __B, __C) __extension__({\ +__builtin_ia32_getmantpd128_mask ((__v2df) __A,\ + (__C << 2) | __B,\ + (__v2df) __W,\ + (__mmask8) __U);\ +}) + +#define _mm_maskz_getmant_pd( __U, __A, __B, __C) __extension__({\ +__builtin_ia32_getmantpd128_mask ((__v2df) __A,\ + (__C << 2) | __B,\ + (__v2df) _mm_setzero_pd (),\ + (__mmask8) __U);\ +}) + +#define _mm256_getmant_pd( __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd256_mask ((__v4df)( __A),\ + (__C << 2) |( __B),\ + (__v4df) _mm256_setzero_pd (),\ + (__mmask8) -1);\ +}) + +#define _mm256_mask_getmant_pd( __W, __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd256_mask ((__v4df)( __A),\ + (__C << 2) |( __B),\ + (__v4df)( __W),\ + (__mmask8)( __U));\ +}) + +#define _mm256_maskz_getmant_pd( __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantpd256_mask ((__v4df)( __A),\ + (__C << 2) |( __B),\ + (__v4df) _mm256_setzero_pd (),\ + (__mmask8)( __U));\ +}) + +#define _mm_getmant_ps( __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps128_mask ((__v4sf)( __A),\ + (__C << 2) |( __B),\ + (__v4sf) _mm_setzero_ps (),\ + (__mmask8) -1);\ +}) + +#define _mm_mask_getmant_ps( __W, __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps128_mask ((__v4sf)( __A),\ + (__C << 2) |( __B),\ + (__v4sf)( __W),\ + (__mmask8)( __U));\ +}) + +#define _mm_maskz_getmant_ps( __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps128_mask ((__v4sf)( __A),\ + (__C << 2) |( __B),\ + (__v4sf) _mm_setzero_ps (),\ + (__mmask8)( __U));\ +}) + +#define _mm256_getmant_ps( __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps256_mask ((__v8sf)( __A),\ + (__C << 2) |( __B),\ + (__v8sf) _mm256_setzero_ps (),\ + (__mmask8) -1);\ +}) + +#define _mm256_mask_getmant_ps( __W, __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps256_mask ((__v8sf)( __A),\ + (__C << 2) |( __B),\ + (__v8sf)( __W),\ + (__mmask8)( __U));\ +}) + +#define _mm256_maskz_getmant_ps( __U, __A, __B, __C) __extension__ ({ \ +__builtin_ia32_getmantps256_mask ((__v8sf)( __A),\ + (__C << 2) |( __B),\ + (__v8sf) _mm256_setzero_ps (),\ + (__mmask8)( __U));\ +}) + #undef __DEFAULT_FN_ATTRS #undef __DEFAULT_FN_ATTRS_BOTH diff --git a/clang/test/CodeGen/avx512f-builtins.c b/clang/test/CodeGen/avx512f-builtins.c index fcda48bd4b48..dc41309a6bb3 100644 --- a/clang/test/CodeGen/avx512f-builtins.c +++ b/clang/test/CodeGen/avx512f-builtins.c @@ -4131,3 +4131,147 @@ __m512i test_mm512_maskz_inserti64x4(__mmask8 __U, __m512i __A, __m256i __B) { // CHECK: @llvm.x86.avx512.mask.inserti64x4 return _mm512_maskz_inserti64x4(__U, __A, __B, 1); } + +__m512d test_mm512_getmant_round_pd(__m512d __A) { + // CHECK-LABEL: @test_mm512_getmant_round_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_getmant_round_pd(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_mask_getmant_round_pd(__m512d __W, __mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_mask_getmant_round_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_mask_getmant_round_pd(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_maskz_getmant_round_pd(__mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_maskz_getmant_round_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_maskz_getmant_round_pd(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_getmant_pd(__m512d __A) { + // CHECK-LABEL: @test_mm512_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_getmant_pd(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512d test_mm512_mask_getmant_pd(__m512d __W, __mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_mask_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_mask_getmant_pd(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512d test_mm512_maskz_getmant_pd(__mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_maskz_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.512 + return _mm512_maskz_getmant_pd(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512 test_mm512_getmant_round_ps(__m512 __A) { + // CHECK-LABEL: @test_mm512_getmant_round_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_getmant_round_ps(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_mask_getmant_round_ps(__m512 __W, __mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_mask_getmant_round_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_mask_getmant_round_ps(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_maskz_getmant_round_ps(__mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_maskz_getmant_round_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_maskz_getmant_round_ps(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_getmant_ps(__m512 __A) { + // CHECK-LABEL: @test_mm512_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_getmant_ps(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512 test_mm512_mask_getmant_ps(__m512 __W, __mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_mask_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_mask_getmant_ps(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512 test_mm512_maskz_getmant_ps(__mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_maskz_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.512 + return _mm512_maskz_getmant_ps(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m512d test_mm512_getexp_round_pd(__m512d __A) { + // CHECK-LABEL: @test_mm512_getexp_round_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_getexp_round_pd(__A, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_mask_getexp_round_pd(__m512d __W, __mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_mask_getexp_round_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_mask_getexp_round_pd(__W, __U, __A, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_maskz_getexp_round_pd(__mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_maskz_getexp_round_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_maskz_getexp_round_pd(__U, __A, _MM_FROUND_CUR_DIRECTION); +} + +__m512d test_mm512_getexp_pd(__m512d __A) { + // CHECK-LABEL: @test_mm512_getexp_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_getexp_pd(__A); +} + +__m512d test_mm512_mask_getexp_pd(__m512d __W, __mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_mask_getexp_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_mask_getexp_pd(__W, __U, __A); +} + +__m512d test_mm512_maskz_getexp_pd(__mmask8 __U, __m512d __A) { + // CHECK-LABEL: @test_mm512_maskz_getexp_pd + // CHECK: @llvm.x86.avx512.mask.getexp.pd.512 + return _mm512_maskz_getexp_pd(__U, __A); +} + +__m512 test_mm512_getexp_round_ps(__m512 __A) { + // CHECK-LABEL: @test_mm512_getexp_round_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_getexp_round_ps(__A, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_mask_getexp_round_ps(__m512 __W, __mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_mask_getexp_round_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_mask_getexp_round_ps(__W, __U, __A, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_maskz_getexp_round_ps(__mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_maskz_getexp_round_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_maskz_getexp_round_ps(__U, __A, _MM_FROUND_CUR_DIRECTION); +} + +__m512 test_mm512_getexp_ps(__m512 __A) { + // CHECK-LABEL: @test_mm512_getexp_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_getexp_ps(__A); +} + +__m512 test_mm512_mask_getexp_ps(__m512 __W, __mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_mask_getexp_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_mask_getexp_ps(__W, __U, __A); +} + +__m512 test_mm512_maskz_getexp_ps(__mmask16 __U, __m512 __A) { + // CHECK-LABEL: @test_mm512_maskz_getexp_ps + // CHECK: @llvm.x86.avx512.mask.getexp.ps.512 + return _mm512_maskz_getexp_ps(__U, __A); +} diff --git a/clang/test/CodeGen/avx512vl-builtins.c b/clang/test/CodeGen/avx512vl-builtins.c index 46487a668264..587c7d2aec82 100644 --- a/clang/test/CodeGen/avx512vl-builtins.c +++ b/clang/test/CodeGen/avx512vl-builtins.c @@ -6190,3 +6190,75 @@ __m256i test_mm256_maskz_inserti32x4(__mmask8 __U, __m256i __A, __m128i __B) { // CHECK: @llvm.x86.avx512.mask.inserti32x4 return _mm256_maskz_inserti32x4(__U, __A, __B, 1); } + +__m128d test_mm_getmant_pd(__m128d __A) { + // CHECK-LABEL: @test_mm_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.128 + return _mm_getmant_pd(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m128d test_mm_mask_getmant_pd(__m128d __W, __mmask8 __U, __m128d __A) { + // CHECK-LABEL: @test_mm_mask_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.128 + return _mm_mask_getmant_pd(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m128d test_mm_maskz_getmant_pd(__mmask8 __U, __m128d __A) { + // CHECK-LABEL: @test_mm_maskz_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.128 + return _mm_maskz_getmant_pd(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256d test_mm256_getmant_pd(__m256d __A) { + // CHECK-LABEL: @test_mm256_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.256 + return _mm256_getmant_pd(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256d test_mm256_mask_getmant_pd(__m256d __W, __mmask8 __U, __m256d __A) { + // CHECK-LABEL: @test_mm256_mask_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.256 + return _mm256_mask_getmant_pd(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256d test_mm256_maskz_getmant_pd(__mmask8 __U, __m256d __A) { + // CHECK-LABEL: @test_mm256_maskz_getmant_pd + // CHECK: @llvm.x86.avx512.mask.getmant.pd.256 + return _mm256_maskz_getmant_pd(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m128 test_mm_getmant_ps(__m128 __A) { + // CHECK-LABEL: @test_mm_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.128 + return _mm_getmant_ps(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m128 test_mm_mask_getmant_ps(__m128 __W, __mmask8 __U, __m128 __A) { + // CHECK-LABEL: @test_mm_mask_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.128 + return _mm_mask_getmant_ps(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m128 test_mm_maskz_getmant_ps(__mmask8 __U, __m128 __A) { + // CHECK-LABEL: @test_mm_maskz_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.128 + return _mm_maskz_getmant_ps(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256 test_mm256_getmant_ps(__m256 __A) { + // CHECK-LABEL: @test_mm256_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.256 + return _mm256_getmant_ps(__A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256 test_mm256_mask_getmant_ps(__m256 __W, __mmask8 __U, __m256 __A) { + // CHECK-LABEL: @test_mm256_mask_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.256 + return _mm256_mask_getmant_ps(__W, __U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +} + +__m256 test_mm256_maskz_getmant_ps(__mmask8 __U, __m256 __A) { + // CHECK-LABEL: @test_mm256_maskz_getmant_ps + // CHECK: @llvm.x86.avx512.mask.getmant.ps.256 + return _mm256_maskz_getmant_ps(__U, __A,_MM_MANT_NORM_p5_2, _MM_MANT_SIGN_nan); +}