Partial revert of r146791; vpermilps/vpermilpd instructions accepts ymm/mem/imm8.

llvm-svn: 146797
This commit is contained in:
Chad Rosier 2011-12-17 00:50:42 +00:00
parent e321795c60
commit 3648646b2b
2 changed files with 12 additions and 8 deletions

View File

@ -425,9 +425,9 @@ BUILTIN(__builtin_ia32_cvttps2dq256, "V8iV8f", "")
BUILTIN(__builtin_ia32_vperm2f128_pd256, "V4dV4dV4dIc", "")
BUILTIN(__builtin_ia32_vperm2f128_ps256, "V8fV8fV8fIc", "")
BUILTIN(__builtin_ia32_vperm2f128_si256, "V8iV8iV8iIc", "")
BUILTIN(__builtin_ia32_vpermilpd, "V2dV2dIc", "")
BUILTIN(__builtin_ia32_vpermilpd, "V2dV2dc", "")
BUILTIN(__builtin_ia32_vpermilps, "V4fV4fc", "")
BUILTIN(__builtin_ia32_vpermilpd256, "V4dV4dIc", "")
BUILTIN(__builtin_ia32_vpermilpd256, "V4dV4dc", "")
BUILTIN(__builtin_ia32_vpermilps256, "V8fV8fc", "")
BUILTIN(__builtin_ia32_vinsertf128_pd256, "V4dV4dV2dIc", "")
BUILTIN(__builtin_ia32_vinsertf128_ps256, "V8fV8fV4fIc", "")

View File

@ -258,13 +258,17 @@ _mm256_permutevar_ps(__m256 a, __m256i c)
(__v8si)c);
}
#define _mm_permute_pd(A, C) __extension__ ({ \
__m128d __A = (A); \
(__m128d)__builtin_ia32_vpermilpd((__v2df)__A, C); })
static __inline __m128d __attribute__((__always_inline__, __nodebug__))
_mm_permute_pd(__m128d a, const int c)
{
return (__m128d)__builtin_ia32_vpermilpd((__v2df)a, c);
}
#define _mm256_permute_pd(A, C) __extension__ ({ \
__m256d __A = (A); \
(__m256d)__builtin_ia32_vpermilpd256((__v4df)__A, C); })
static __inline __m256d __attribute__((__always_inline__, __nodebug__))
_mm256_permute_pd(__m256d a, const int c)
{
return (__m256d)__builtin_ia32_vpermilpd256((__v4df)a, c);
}
static __inline __m128 __attribute__((__always_inline__, __nodebug__))
_mm_permute_ps(__m128 a, const int c)