This is an archive of the discontinued LLVM Phabricator instance.

Differential D19326

[Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp and getmant instruction set
ClosedPublic

Authored by m_zuckerman on Apr 20 2016, 8:25 AM.

Details

Reviewers
AsafBadouh
delena
igorb
Commits
rGa1ceca20b679: [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp…
rC267129: [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp…
rL267129: [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp…

Diff Detail

Repository
rL LLVM

Event Timeline

m_zuckerman updated this revision to Diff 54374.Apr 20 2016, 8:25 AM
m_zuckerman updated this revision to Diff 54375.
m_zuckerman retitled this revision from to [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp and getmant .
m_zuckerman updated this object.
m_zuckerman added reviewers: AsafBadouh, igorb, delena.
m_zuckerman added a subscriber: llvm-commits.
m_zuckerman updated this revision to Diff 54376.Apr 20 2016, 8:28 AM
m_zuckerman retitled this revision from [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp and getmant to [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp and getmant instruction set.Apr 20 2016, 8:37 AM
igorb accepted this revision.Apr 20 2016, 12:06 PM
igorb edited edge metadata.

LGTM

This revision is now accepted and ready to land.Apr 20 2016, 12:06 PM
Closed by commit rL267129: [Clang][AVX512][BUILTIN] Adding scalar intrinsics for rsqrt14 ,rcp14, getexp… (authored by mzuckerm). · Explain WhyApr 22 2016, 3:11 AM
This revision was automatically updated to reflect the committed changes.

Revision Contents

PathSize
cfe/
trunk/
lib/
Headers/
215 lines
test/
CodeGen/
146 lines

Diff 54622

cfe/trunk/lib/Headers/avx512fintrin.h

Show First 20 Lines • Show All 1,015 Lines • ▼ Show 20 Lines
{ {
return (__m128) __builtin_ia32_rsqrt14ss_mask ((__v4sf) __A, return (__m128) __builtin_ia32_rsqrt14ss_mask ((__v4sf) __A,
(__v4sf) __B, (__v4sf) __B,
(__v4sf) (__v4sf)
_mm_setzero_ps (), _mm_setzero_ps (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_mask_rsqrt14_ss (__m128 __W, __mmask8 __U, __m128 __A, __m128 __B)
{
return (__m128) __builtin_ia32_rsqrt14ss_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) __W,
(__mmask8) __U);
}
static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_maskz_rsqrt14_ss (__mmask8 __U, __m128 __A, __m128 __B)
{
return (__m128) __builtin_ia32_rsqrt14ss_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) _mm_setzero_ps (),
(__mmask8) __U);
}
static __inline__ __m128d __DEFAULT_FN_ATTRS static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_rsqrt14_sd(__m128d __A, __m128d __B) _mm_rsqrt14_sd(__m128d __A, __m128d __B)
{ {
return (__m128d) __builtin_ia32_rsqrt14sd_mask ((__v2df) __A, return (__m128d) __builtin_ia32_rsqrt14sd_mask ((__v2df) __A,
(__v2df) __B, (__v2df) __B,
(__v2df) (__v2df)
_mm_setzero_pd (), _mm_setzero_pd (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_mask_rsqrt14_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_rsqrt14sd_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) __W,
(__mmask8) __U);
}
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_maskz_rsqrt14_sd (__mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_rsqrt14sd_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) _mm_setzero_pd (),
(__mmask8) __U);
}
static __inline__ __m512d __DEFAULT_FN_ATTRS static __inline__ __m512d __DEFAULT_FN_ATTRS
_mm512_rcp14_pd(__m512d __A) _mm512_rcp14_pd(__m512d __A)
{ {
return (__m512d) __builtin_ia32_rcp14pd512_mask ((__v8df) __A, return (__m512d) __builtin_ia32_rcp14pd512_mask ((__v8df) __A,
(__v8df) (__v8df)
_mm512_setzero_pd (), _mm512_setzero_pd (),
(__mmask8) -1); (__mmask8) -1);
} }
Show All 11 Lines
{ {
return (__m128) __builtin_ia32_rcp14ss_mask ((__v4sf) __A, return (__m128) __builtin_ia32_rcp14ss_mask ((__v4sf) __A,
(__v4sf) __B, (__v4sf) __B,
(__v4sf) (__v4sf)
_mm_setzero_ps (), _mm_setzero_ps (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_mask_rcp14_ss (__m128 __W, __mmask8 __U, __m128 __A, __m128 __B)
{
return (__m128) __builtin_ia32_rcp14ss_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) __W,
(__mmask8) __U);
}
static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_maskz_rcp14_ss (__mmask8 __U, __m128 __A, __m128 __B)
{
return (__m128) __builtin_ia32_rcp14ss_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) _mm_setzero_ps (),
(__mmask8) __U);
}
static __inline__ __m128d __DEFAULT_FN_ATTRS static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_rcp14_sd(__m128d __A, __m128d __B) _mm_rcp14_sd(__m128d __A, __m128d __B)
{ {
return (__m128d) __builtin_ia32_rcp14sd_mask ((__v2df) __A, return (__m128d) __builtin_ia32_rcp14sd_mask ((__v2df) __A,
(__v2df) __B, (__v2df) __B,
(__v2df) (__v2df)
_mm_setzero_pd (), _mm_setzero_pd (),
(__mmask8) -1); (__mmask8) -1);
} }
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_mask_rcp14_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_rcp14sd_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) __W,
(__mmask8) __U);
}
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_maskz_rcp14_sd (__mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_rcp14sd_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) _mm_setzero_pd (),
(__mmask8) __U);
}
static __inline __m512 __DEFAULT_FN_ATTRS static __inline __m512 __DEFAULT_FN_ATTRS
_mm512_floor_ps(__m512 __A) _mm512_floor_ps(__m512 __A)
{ {
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A, return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A,
_MM_FROUND_FLOOR, _MM_FROUND_FLOOR,
(__v16sf) __A, -1, (__v16sf) __A, -1,
_MM_FROUND_CUR_DIRECTION); _MM_FROUND_CUR_DIRECTION);
} }
▲ Show 20 Lines • Show All 2,924 Lines • ▼ Show 20 Lines
static __inline__ __m128d __DEFAULT_FN_ATTRS static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_getexp_sd (__m128d __A, __m128d __B) _mm_getexp_sd (__m128d __A, __m128d __B)
{ {
return (__m128d) __builtin_ia32_getexpsd128_round_mask ((__v2df) __A, return (__m128d) __builtin_ia32_getexpsd128_round_mask ((__v2df) __A,
(__v2df) __B, (__v2df) _mm_setzero_pd(), (__mmask8) -1, _MM_FROUND_CUR_DIRECTION); (__v2df) __B, (__v2df) _mm_setzero_pd(), (__mmask8) -1, _MM_FROUND_CUR_DIRECTION);
} }
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_mask_getexp_sd (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_getexpsd128_round_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) __W,
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
#define _mm_mask_getexp_round_sd( __W, __U, __A, __B, __R) __extension__ ({\
__builtin_ia32_getexpsd128_round_mask ((__v2df) __A,\
(__v2df) __B,\
(__v2df) __W,\
(__mmask8) __U,\
__R);\
})
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_maskz_getexp_sd (__mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_getexpsd128_round_mask ( (__v2df) __A,
(__v2df) __B,
(__v2df) _mm_setzero_pd (),
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
#define _mm_maskz_getexp_round_sd( __U, __A, __B, __R) __extension__ ({\
__builtin_ia32_getexpsd128_round_mask ( (__v2df) __A,\
(__v2df) __B,\
(__v2df) _mm_setzero_pd (),\
(__mmask8) __U,\
__R);\
})
#define _mm_getexp_round_ss( __A, __B, __R) __extension__ ({ \ #define _mm_getexp_round_ss( __A, __B, __R) __extension__ ({ \
__builtin_ia32_getexpss128_round_mask ((__v4sf)( __A),\ __builtin_ia32_getexpss128_round_mask ((__v4sf)( __A),\
(__v4sf)( __B), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\ (__v4sf)( __B), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\
( __R));\ ( __R));\
}) })
static __inline__ __m128 __DEFAULT_FN_ATTRS static __inline__ __m128 __DEFAULT_FN_ATTRS
_mm_getexp_ss (__m128 __A, __m128 __B) _mm_getexp_ss (__m128 __A, __m128 __B)
{ {
return (__m128) __builtin_ia32_getexpss128_round_mask ((__v4sf) __A, return (__m128) __builtin_ia32_getexpss128_round_mask ((__v4sf) __A,
(__v4sf) __B, (__v4sf) _mm_setzero_ps(), (__mmask8) -1, _MM_FROUND_CUR_DIRECTION); (__v4sf) __B, (__v4sf) _mm_setzero_ps(), (__mmask8) -1, _MM_FROUND_CUR_DIRECTION);
} }
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_mask_getexp_ss (__m128d __W, __mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_getexpss128_round_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) __W,
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
#define _mm_mask_getexp_round_ss( __W, __U, __A, __B, __R) __extension__ ({\
__builtin_ia32_getexpss128_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(__v4sf) __W,\
(__mmask8) __U,\
__R);\
})
static __inline__ __m128d __DEFAULT_FN_ATTRS
_mm_maskz_getexp_ss (__mmask8 __U, __m128d __A, __m128d __B)
{
return (__m128d) __builtin_ia32_getexpss128_round_mask ((__v4sf) __A,
(__v4sf) __B,
(__v4sf) _mm_setzero_pd (),
(__mmask8) __U,
_MM_FROUND_CUR_DIRECTION);
}
#define _mm_maskz_getexp_round_ss( __U, __A, __B, __R) __extension__ ({\
__builtin_ia32_getexpss128_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(__v4sf) _mm_setzero_ps (),\
(__mmask8) __U,\
__R);\
})
#define _mm_getmant_round_sd( __A, __B, __C, __D, __R) __extension__ ({ \ #define _mm_getmant_round_sd( __A, __B, __C, __D, __R) __extension__ ({ \
__builtin_ia32_getmantsd_round_mask ((__v2df)( __A),\ __builtin_ia32_getmantsd_round_mask ((__v2df)( __A),\
(__v2df)( __B),\ (__v2df)( __B),\
(( __D) << 2) |( __C), (__v2df) _mm_setzero_pd(), (__mmask8) -1,\ (( __D) << 2) |( __C), (__v2df) _mm_setzero_pd(), (__mmask8) -1,\
( __R));\ ( __R));\
}) })
#define _mm_getmant_sd( __A, __B, __C, __D) __extension__ ({ \ #define _mm_getmant_sd( __A, __B, __C, __D) __extension__ ({ \
__builtin_ia32_getmantsd_round_mask ((__v2df)( __A),\ __builtin_ia32_getmantsd_round_mask ((__v2df)( __A),\
(__v2df)( __B),\ (__v2df)( __B),\
(( __D) << 2) |( __C), (__v2df) _mm_setzero_pd(), (__mmask8) -1,\ (( __D) << 2) |( __C), (__v2df) _mm_setzero_pd(), (__mmask8) -1,\
_MM_FROUND_CUR_DIRECTION);\ _MM_FROUND_CUR_DIRECTION);\
}) })
#define _mm_mask_getmant_sd( __W, __U, __A, __B, __C, __D) __extension__ ({\
__builtin_ia32_getmantsd_round_mask ( (__v2df) __A,\
(__v2df) __B,\
(( __D) << 2) |( __C),\
(__v2df) __W,\
(__mmask8) __U,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm_mask_getmant_round_sd( __W, __U, __A, __B, __C, __D, __R)({\
__builtin_ia32_getmantsd_round_mask ( (__v2df) __A,\
(__v2df) __B,\
(( __D) << 2) |( __C),\
(__v2df) __W,\
(__mmask8) __U,\
__R);\
})
#define _mm_maskz_getmant_sd( __U, __A, __B, __C, __D) __extension__ ({\
__builtin_ia32_getmantsd_round_mask ( (__v2df) __A,\
(__v2df) __B,\
(( __D) << 2) |( __C),\
(__v2df) _mm_setzero_pd (),\
(__mmask8) __U,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm_maskz_getmant_round_sd( __U, __A, __B, __C, __D, __R) __extension__ ({\
__builtin_ia32_getmantsd_round_mask ( (__v2df) __A,\
(__v2df) __B,\
(( __D) << 2) |( __C),\
(__v2df) _mm_setzero_pd (),\
(__mmask8) __U,\
__R);\
})
#define _mm_getmant_round_ss( __A, __B, __C, __D, __R) __extension__ ({ \ #define _mm_getmant_round_ss( __A, __B, __C, __D, __R) __extension__ ({ \
__builtin_ia32_getmantss_round_mask ((__v4sf)( __A),\ __builtin_ia32_getmantss_round_mask ((__v4sf)( __A),\
(__v4sf)( __B),\ (__v4sf)( __B),\
((__D) << 2) |( __C), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\ ((__D) << 2) |( __C), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\
( __R));\ ( __R));\
}) })
#define _mm_getmant_ss(__A, __B, __C, __D) __extension__ ({ \ #define _mm_getmant_ss(__A, __B, __C, __D) __extension__ ({ \
__builtin_ia32_getmantss_round_mask ((__v4sf)( __A),\ __builtin_ia32_getmantss_round_mask ((__v4sf)( __A),\
(__v4sf)( __B),\ (__v4sf)( __B),\
((__D) << 2) |( __C), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\ ((__D) << 2) |( __C), (__v4sf) _mm_setzero_ps(), (__mmask8) -1,\
_MM_FROUND_CUR_DIRECTION);\ _MM_FROUND_CUR_DIRECTION);\
}) })
#define _mm_mask_getmant_ss( __W, __U, __A, __B, __C, __D) __extension__ ({\
__builtin_ia32_getmantss_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(( __D) << 2) |( __C),\
(__v4sf) __W,\
(__mmask8) __U,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm_mask_getmant_round_ss( __W, __U, __A, __B, __C, __D, __R)({\
__builtin_ia32_getmantss_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(( __D) << 2) |( __C),\
(__v4sf) __W,\
(__mmask8) __U,\
__R);\
})
#define _mm_maskz_getmant_ss( __U, __A, __B, __C, __D) __extension__ ({\
__builtin_ia32_getmantss_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(( __D) << 2) |( __C),\
(__v4sf) _mm_setzero_pd (),\
(__mmask8) __U,\
_MM_FROUND_CUR_DIRECTION);\
})
#define _mm_maskz_getmant_round_ss( __U, __A, __B, __C, __D, __R) __extension__ ({\
__builtin_ia32_getmantss_round_mask ((__v4sf) __A,\
(__v4sf) __B,\
(( __D) << 2) |( __C),\
(__v4sf) _mm_setzero_ps (),\
(__mmask8) __U,\
__R);\
})
static __inline__ __mmask16 __DEFAULT_FN_ATTRS static __inline__ __mmask16 __DEFAULT_FN_ATTRS
_mm512_kmov (__mmask16 __A) _mm512_kmov (__mmask16 __A)
{ {
return __A; return __A;
} }
#define _mm_comi_round_sd(__A, __B, __P, __R) __extension__ ({\ #define _mm_comi_round_sd(__A, __B, __P, __R) __extension__ ({\
▲ Show 20 Lines • Show All 2,348 Lines • Show Last 20 Lines

cfe/trunk/test/CodeGen/avx512f-builtins.c

Show First 20 Lines • Show All 2,550 Lines • ▼ Show 20 Lines
} }
__m128d test_mm_getmant_sd(__m128d __A, __m128d __B) { __m128d test_mm_getmant_sd(__m128d __A, __m128d __B) {
// CHECK-LABEL: @test_mm_getmant_sd // CHECK-LABEL: @test_mm_getmant_sd
// CHECK: @llvm.x86.avx512.mask.getmant.sd // CHECK: @llvm.x86.avx512.mask.getmant.sd
return _mm_getmant_sd(__A, __B, _MM_MANT_NORM_1_2, _MM_MANT_SIGN_src); return _mm_getmant_sd(__A, __B, _MM_MANT_NORM_1_2, _MM_MANT_SIGN_src);
} }
__m128 test_mm_getmant_round_ss(__m128 __A, __m128 __B) { __m128 test_mm_getmant_round_ss(__m128 __A, __m128 __B) {
// CHECK-LABEL: @test_mm_getmant_round_ss // CHECK-LABEL: @test_mm_getmant_round_ss
// CHECK: @llvm.x86.avx512.mask.getmant.ss // CHECK: @llvm.x86.avx512.mask.getmant.ss
return _mm_getmant_round_ss(__A, __B, _MM_MANT_NORM_1_2, _MM_MANT_SIGN_src, 8); return _mm_getmant_round_ss(__A, __B, _MM_MANT_NORM_1_2, _MM_MANT_SIGN_src, 8);
} }
__m128 test_mm_getmant_ss(__m128 __A, __m128 __B) { __m128 test_mm_getmant_ss(__m128 __A, __m128 __B) {
// CHECK-LABEL: @test_mm_getmant_ss // CHECK-LABEL: @test_mm_getmant_ss
▲ Show 20 Lines • Show All 1,798 Lines • ▼ Show 20 Lines
} }
__m512i test_mm512_mask_i32gather_epi64(__m512i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) { __m512i test_mm512_mask_i32gather_epi64(__m512i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
// CHECK-LABEL: @test_mm512_mask_i32gather_epi64 // CHECK-LABEL: @test_mm512_mask_i32gather_epi64
// CHECK: @llvm.x86.avx512.gather.dpq.512 // CHECK: @llvm.x86.avx512.gather.dpq.512
return _mm512_mask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2); return _mm512_mask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2);
} }
__m128d test_mm_mask_rsqrt14_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_rsqrt14_sd
// CHECK: @llvm.x86.avx512.rsqrt14.sd
return _mm_mask_rsqrt14_sd(__W, __U, __A, __B);
}
__m128d test_mm_maskz_rsqrt14_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_rsqrt14_sd
// CHECK: @llvm.x86.avx512.rsqrt14.sd
return _mm_maskz_rsqrt14_sd(__U, __A, __B);
}
__m128 test_mm_mask_rsqrt14_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_rsqrt14_ss
// CHECK: @llvm.x86.avx512.rsqrt14.ss
return _mm_mask_rsqrt14_ss(__W, __U, __A, __B);
}
__m128 test_mm_maskz_rsqrt14_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_rsqrt14_ss
// CHECK: @llvm.x86.avx512.rsqrt14.ss
return _mm_maskz_rsqrt14_ss(__U, __A, __B);
}
__m128d test_mm_mask_rcp14_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_rcp14_sd
// CHECK: @llvm.x86.avx512.rcp14.sd
return _mm_mask_rcp14_sd(__W, __U, __A, __B);
}
__m128d test_mm_maskz_rcp14_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_rcp14_sd
// CHECK: @llvm.x86.avx512.rcp14.sd
return _mm_maskz_rcp14_sd(__U, __A, __B);
}
__m128 test_mm_mask_rcp14_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_rcp14_ss
// CHECK: @llvm.x86.avx512.rcp14.ss
return _mm_mask_rcp14_ss(__W, __U, __A, __B);
}
__m128 test_mm_maskz_rcp14_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_rcp14_ss
// CHECK: @llvm.x86.avx512.rcp14.ss
return _mm_maskz_rcp14_ss(__U, __A, __B);
}
__m128d test_mm_mask_getexp_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_getexp_sd
// CHECK: @llvm.x86.avx512.mask.getexp.sd
return _mm_mask_getexp_sd(__W, __U, __A, __B);
}
__m128d test_mm_mask_getexp_round_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_getexp_round_sd
// CHECK: @llvm.x86.avx512.mask.getexp.sd
return _mm_mask_getexp_round_sd(__W, __U, __A, __B, _MM_FROUND_CUR_DIRECTION);
}
__m128d test_mm_maskz_getexp_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_getexp_sd
// CHECK: @llvm.x86.avx512.mask.getexp.sd
return _mm_maskz_getexp_sd(__U, __A, __B);
}
__m128d test_mm_maskz_getexp_round_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_getexp_round_sd
// CHECK: @llvm.x86.avx512.mask.getexp.sd
return _mm_maskz_getexp_round_sd(__U, __A, __B, _MM_FROUND_CUR_DIRECTION);
}
__m128 test_mm_mask_getexp_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_getexp_ss
// CHECK: @llvm.x86.avx512.mask.getexp.ss
return _mm_mask_getexp_ss(__W, __U, __A, __B);
}
__m128 test_mm_mask_getexp_round_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_getexp_round_ss
// CHECK: @llvm.x86.avx512.mask.getexp.ss
return _mm_mask_getexp_round_ss(__W, __U, __A, __B, _MM_FROUND_CUR_DIRECTION);
}
__m128 test_mm_maskz_getexp_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_getexp_ss
// CHECK: @llvm.x86.avx512.mask.getexp.ss
return _mm_maskz_getexp_ss(__U, __A, __B);
}
__m128 test_mm_maskz_getexp_round_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_getexp_round_ss
// CHECK: @llvm.x86.avx512.mask.getexp.ss
return _mm_maskz_getexp_round_ss(__U, __A, __B, _MM_FROUND_CUR_DIRECTION);
}
__m128d test_mm_mask_getmant_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_getmant_sd
// CHECK: @llvm.x86.avx512.mask.getmant.sd
return _mm_mask_getmant_sd(__W, __U, __A, __B, 1, 2);
}
__m128d test_mm_mask_getmant_round_sd(__m128d __W, __mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_mask_getmant_round_sd
// CHECK: @llvm.x86.avx512.mask.getmant.sd
return _mm_mask_getmant_round_sd(__W, __U, __A, __B, 1, 2, _MM_FROUND_CUR_DIRECTION);
}
__m128d test_mm_maskz_getmant_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_getmant_sd
// CHECK: @llvm.x86.avx512.mask.getmant.sd
return _mm_maskz_getmant_sd(__U, __A, __B, 1, 2);
}
__m128d test_mm_maskz_getmant_round_sd(__mmask8 __U, __m128d __A, __m128d __B){
// CHECK-LABEL: @test_mm_maskz_getmant_round_sd
// CHECK: @llvm.x86.avx512.mask.getmant.sd
return _mm_maskz_getmant_round_sd(__U, __A, __B, 1, 2, _MM_FROUND_CUR_DIRECTION);
}
__m128 test_mm_mask_getmant_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_getmant_ss
// CHECK: @llvm.x86.avx512.mask.getmant.ss
return _mm_mask_getmant_ss(__W, __U, __A, __B, 1, 2);
}
__m128 test_mm_mask_getmant_round_ss(__m128 __W, __mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_mask_getmant_round_ss
// CHECK: @llvm.x86.avx512.mask.getmant.ss
return _mm_mask_getmant_round_ss(__W, __U, __A, __B, 1, 2, _MM_FROUND_CUR_DIRECTION);
}
__m128 test_mm_maskz_getmant_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_getmant_ss
// CHECK: @llvm.x86.avx512.mask.getmant.ss
return _mm_maskz_getmant_ss(__U, __A, __B, 1, 2);
}
__m128 test_mm_maskz_getmant_round_ss(__mmask8 __U, __m128 __A, __m128 __B){
// CHECK-LABEL: @test_mm_maskz_getmant_round_ss
// CHECK: @llvm.x86.avx512.mask.getmant.ss
return _mm_maskz_getmant_round_ss(__U, __A, __B, 1, 2, _MM_FROUND_CUR_DIRECTION);
}