From b738d9533018763e00f7728a4242535d346adc0c Mon Sep 17 00:00:00 2001 From: Jason Volk Date: Tue, 8 Sep 2020 00:46:38 -0700 Subject: [PATCH] ircd::simd: Remove precocious 512-shift intrinsic templates. --- include/ircd/simd/shift.h | 34 ---------------------------------- 1 file changed, 34 deletions(-) diff --git a/include/ircd/simd/shift.h b/include/ircd/simd/shift.h index 72c157f6f..3f6ade86f 100644 --- a/include/ircd/simd/shift.h +++ b/include/ircd/simd/shift.h @@ -147,22 +147,6 @@ noexcept } #endif -#if defined(HAVE_X86INTRIN_H) && defined(__AVX512F__) -template -[[using gnu: always_inline, gnu_inline, artificial]] -extern inline typename std::enable_if::type -ircd::simd::shr(const T a) -noexcept -{ - static_assert - ( - b % 8 == 0, "ymmx register only shifts right at bytewise resolution." - ); - - return T(_mm512_srli_si512(u512x1(a), b / 8)); -} -#else template [[using gnu: always_inline, gnu_inline, artificial]] @@ -172,24 +156,7 @@ noexcept { return _shr(a); } -#endif -#if defined(HAVE_X86INTRIN_H) && defined(__AVX512F__) -template -[[using gnu: always_inline, gnu_inline, artificial]] -extern inline typename std::enable_if::type -ircd::simd::shl(const T a) -noexcept -{ - static_assert - ( - b % 8 == 0, "ymmx register only shifts left at bytewise resolution." - ); - - return T(_mm512_slli_si512(u512x1(a), b / 8)); -} -#else template [[using gnu: always_inline, gnu_inline, artificial]] @@ -199,7 +166,6 @@ noexcept { return _shl(a); } -#endif template