mirror of
https://github.com/matrix-construct/construct
synced 2024-07-05 18:18:35 +02:00
105 lines
2.5 KiB
C++
105 lines
2.5 KiB
C++
// The Construct
|
|
//
|
|
// Copyright (C) The Construct Developers, Authors & Contributors
|
|
// Copyright (C) 2016-2020 Jason Volk <jason@zemos.net>
|
|
//
|
|
// Permission to use, copy, modify, and/or distribute this software for any
|
|
// purpose with or without fee is hereby granted, provided that the above
|
|
// copyright notice and this permission notice is present in all copies. The
|
|
// full license for this software is available in the LICENSE file.
|
|
|
|
#pragma once
|
|
#define HAVE_IRCD_SIMD_SHIFT_H
|
|
|
|
// xmmx shifter workarounds
|
|
namespace ircd::simd
|
|
{
|
|
template<int b,
|
|
class T>
|
|
typename std::enable_if<sizeof(T) == 16, T>::type
|
|
shl(const T a) noexcept;
|
|
|
|
template<int b,
|
|
class T>
|
|
typename std::enable_if<sizeof(T) == 32, T>::type
|
|
shl(const T a) noexcept;
|
|
|
|
template<int b,
|
|
class T>
|
|
typename std::enable_if<sizeof(T) == 16, T>::type
|
|
shr(const T a) noexcept;
|
|
|
|
template<int b,
|
|
class T>
|
|
typename std::enable_if<sizeof(T) == 32, T>::type
|
|
shr(const T a) noexcept;
|
|
}
|
|
|
|
#ifdef HAVE_X86INTRIN_H
|
|
template<int b,
|
|
class T>
|
|
[[using gnu: always_inline, gnu_inline, artificial]]
|
|
extern inline typename std::enable_if<sizeof(T) == 16, T>::type
|
|
ircd::simd::shr(const T a)
|
|
noexcept
|
|
{
|
|
static_assert
|
|
(
|
|
b % 8 == 0, "xmmx register only shifts right at bytewise resolution."
|
|
);
|
|
|
|
return T(_mm_bsrli_si128(u128x1(a), b / 8));
|
|
}
|
|
#endif
|
|
|
|
#ifdef HAVE_X86INTRIN_H
|
|
template<int b,
|
|
class T>
|
|
[[using gnu: always_inline, gnu_inline, artificial]]
|
|
extern inline typename std::enable_if<sizeof(T) == 16, T>::type
|
|
ircd::simd::shl(const T a)
|
|
noexcept
|
|
{
|
|
static_assert
|
|
(
|
|
b % 8 == 0, "xmmx register only shifts left at bytewise resolution."
|
|
);
|
|
|
|
return T(_mm_bslli_si128(u128x1(a), b / 8));
|
|
}
|
|
#endif
|
|
|
|
#if defined(HAVE_X86INTRIN_H) && defined(__AVX2__)
|
|
template<int b,
|
|
class T>
|
|
[[using gnu: always_inline, gnu_inline, artificial]]
|
|
extern inline typename std::enable_if<sizeof(T) == 32, T>::type
|
|
ircd::simd::shr(const T a)
|
|
noexcept
|
|
{
|
|
static_assert
|
|
(
|
|
b % 8 == 0, "ymmx register only shifts right at bytewise resolution."
|
|
);
|
|
|
|
return T(_mm256_srli_si256(u256x1(a), b / 8));
|
|
}
|
|
#endif
|
|
|
|
#if defined(HAVE_X86INTRIN_H) && defined(__AVX2__)
|
|
template<int b,
|
|
class T>
|
|
[[using gnu: always_inline, gnu_inline, artificial]]
|
|
extern inline typename std::enable_if<sizeof(T) == 32, T>::type
|
|
ircd::simd::shl(const T a)
|
|
noexcept
|
|
{
|
|
static_assert
|
|
(
|
|
b % 8 == 0, "ymmx register only shifts left at bytewise resolution."
|
|
);
|
|
|
|
return T(_mm256_slli_si256(u256x1(a), b / 8));
|
|
}
|
|
#endif
|