diff options
| author | Chad Rosier <mcrosier@apple.com> | 2011-12-17 00:50:42 +0000 |
|---|---|---|
| committer | Chad Rosier <mcrosier@apple.com> | 2011-12-17 00:50:42 +0000 |
| commit | 197808762de70edd67be1e4adbcc6cfc1823f53a (patch) | |
| tree | 33d4a5075538e80bffc1f6752f36e78961911d56 | |
| parent | fc038e9ef8ed262724f42597ca5c844de97b1202 (diff) | |
Partial revert of r146791; vpermilps/vpermilpd instructions accepts ymm/mem/imm8.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@146797 91177308-0d34-0410-b5e6-96231b3b80d8
| -rw-r--r-- | include/clang/Basic/BuiltinsX86.def | 4 | ||||
| -rw-r--r-- | lib/Headers/avxintrin.h | 16 |
2 files changed, 12 insertions, 8 deletions
diff --git a/include/clang/Basic/BuiltinsX86.def b/include/clang/Basic/BuiltinsX86.def index 8262b3e6a5..88aaf67974 100644 --- a/include/clang/Basic/BuiltinsX86.def +++ b/include/clang/Basic/BuiltinsX86.def @@ -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", "") diff --git a/lib/Headers/avxintrin.h b/lib/Headers/avxintrin.h index ea26fa575f..bb32462736 100644 --- a/lib/Headers/avxintrin.h +++ b/lib/Headers/avxintrin.h @@ -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) |