Add XOP frcz instrinsics.

llvm-svn: 158492
This commit is contained in:
Craig Topper 2012-06-15 06:33:42 +00:00
parent 1f8b48ebb1
commit 9e28bf9345
3 changed files with 72 additions and 0 deletions

View File

@ -701,5 +701,11 @@ BUILTIN(__builtin_ia32_vpermil2pd, "V2dV2dV2dV2LLiIc", "")
BUILTIN(__builtin_ia32_vpermil2pd256, "V4dV4dV4dV4LLiIc", "")
BUILTIN(__builtin_ia32_vpermil2ps, "V4fV4fV4fV4iIc", "")
BUILTIN(__builtin_ia32_vpermil2ps256, "V8fV8fV8fV8iIc", "")
BUILTIN(__builtin_ia32_vfrczss, "V4fV4f", "")
BUILTIN(__builtin_ia32_vfrczsd, "V2dV2d", "")
BUILTIN(__builtin_ia32_vfrczps, "V4fV4f", "")
BUILTIN(__builtin_ia32_vfrczpd, "V2dV2d", "")
BUILTIN(__builtin_ia32_vfrczps256, "V8fV8f", "")
BUILTIN(__builtin_ia32_vfrczpd256, "V4dV4d", "")
#undef BUILTIN

View File

@ -370,6 +370,42 @@ _mm_sha_epi64(__m128i __A, __m128i __B)
(__m256)__builtin_ia32_vpermil2ps256((__v8sf)__X, (__v8sf)__Y, \
(__v8si)__C, (I)); })
static __inline__ __m128 __attribute__((__always_inline__, __nodebug__))
_mm_frcz_ss(__m128 __A)
{
return (__m128)__builtin_ia32_vfrczss((__v4sf)__A);
}
static __inline__ __m128d __attribute__((__always_inline__, __nodebug__))
_mm_frcz_sd(__m128d __A)
{
return (__m128d)__builtin_ia32_vfrczsd((__v2df)__A);
}
static __inline__ __m128 __attribute__((__always_inline__, __nodebug__))
_mm_frcz_ps(__m128 __A)
{
return (__m128)__builtin_ia32_vfrczps((__v4sf)__A);
}
static __inline__ __m128d __attribute__((__always_inline__, __nodebug__))
_mm_frcz_pd(__m128d __A)
{
return (__m128d)__builtin_ia32_vfrczpd((__v2df)__A);
}
static __inline__ __m256 __attribute__((__always_inline__, __nodebug__))
_mm_frcz_ps(__m256 __A)
{
return (__m256)__builtin_ia32_vfrczps((__v4sf)__A);
}
static __inline__ __m256d __attribute__((__always_inline__, __nodebug__))
_mm_frcz_pd(__m256d __A)
{
return (__m256d)__builtin_ia32_vfrczpd((__v2df)__A);
}
#endif /* __XOP__ */
#endif /* __XOPINTRIN_H */

View File

@ -294,3 +294,33 @@ __m256 test_mm256_permute2_ps(__m256 a, __m256 b, __m256i c) {
// CHECK: @llvm.x86.xop.vpermil2ps.256
return _mm256_permute2_ps(a, b, c, 0);
}
__m128 test_mm_frcz_ss(__m128 a) {
// CHECK: @llvm.x86.xop.vfrcz.ss
return _mm_frcz_ss(a);
}
__m128d test_mm_frcz_sd(__m128d a) {
// CHECK: @llvm.x86.xop.vfrcz.sd
return _mm_frcz_sd(a);
}
__m128 test_mm_frcz_ps(__m128 a) {
// CHECK: @llvm.x86.xop.vfrcz.ps
return _mm_frcz_ps(a);
}
__m128d test_mm_frcz_pd(__m128d a) {
// CHECK: @llvm.x86.xop.vfrcz.pd
return _mm_frcz_pd(a);
}
__m256 test_mm256_frcz_ps(__m256 a) {
// CHECK: @llvm.x86.xop.vfrcz.ps.256
return _mm256_frcz_ps(a);
}
__m256d test_mm256_frcz_pd(__m256d a) {
// CHECK: @llvm.x86.xop.vfrcz.pd.256
return _mm256_frcz_pd(a);
}