Botan 2.19.2
Crypto and TLS for C&
Public Member Functions | Static Public Member Functions | List of all members
Botan::SIMD_8x32 Class Referencefinal

#include <simd_avx2.h>

Public Member Functions

SIMD_8x32 andc (const SIMD_8x32 &other) const
 
__m256i BOTAN_FUNC_ISA ("avx2") handle() const
 
template<size_t ROT1, size_t ROT2, size_t ROT3>
SIMD_8x32 BOTAN_FUNC_ISA ("avx2") rho() const
 
template<int SHIFT>
 BOTAN_FUNC_ISA ("avx2") SIMD_8x32 shl() const
 
template<int SHIFT>
 BOTAN_FUNC_ISA ("avx2") SIMD_8x32 shr() const
 
SIMD_8x32 bswap () const
 
SIMD_8x32 operator& (const SIMD_8x32 &other) const
 
void operator&= (const SIMD_8x32 &other)
 
SIMD_8x32 operator+ (const SIMD_8x32 &other) const
 
void operator+= (const SIMD_8x32 &other)
 
SIMD_8x32 operator- (const SIMD_8x32 &other) const
 
void operator-= (const SIMD_8x32 &other)
 
SIMD_8x32 & operator= (const SIMD_8x32 &other)=default
 
SIMD_8x32 & operator= (SIMD_8x32 &&other)=default
 
SIMD_8x32 operator^ (const SIMD_8x32 &other) const
 
void operator^= (const SIMD_8x32 &other)
 
SIMD_8x32 operator| (const SIMD_8x32 &other) const
 
void operator|= (const SIMD_8x32 &other)
 
SIMD_8x32 operator~ () const
 
template<size_t ROT>
SIMD_8x32 rotl () const
 
template<size_t ROT>
SIMD_8x32 rotr () const
 
BOTAN_FORCE_INLINE SIMD_8x32 ()
 
 SIMD_8x32 (__m256i x)
 
 SIMD_8x32 (const SIMD_8x32 &other)=default
 
 SIMD_8x32 (const uint32_t B[8])
 
 SIMD_8x32 (SIMD_8x32 &&other)=default
 
 SIMD_8x32 (uint32_t B0, uint32_t B1, uint32_t B2, uint32_t B3, uint32_t B4, uint32_t B5, uint32_t B6, uint32_t B7)
 
void store_be (uint8_t out[]) const
 
void store_le (uint8_t out[]) const
 

Static Public Member Functions

static SIMD_8x32 load_be (const uint8_t *in)
 
static SIMD_8x32 load_le (const uint8_t *in)
 
static void reset_registers ()
 
static SIMD_8x32 splat (uint32_t B)
 
static void transpose (SIMD_8x32 &B0, SIMD_8x32 &B1, SIMD_8x32 &B2, SIMD_8x32 &B3)
 
static void transpose (SIMD_8x32 &B0, SIMD_8x32 &B1, SIMD_8x32 &B2, SIMD_8x32 &B3, SIMD_8x32 &B4, SIMD_8x32 &B5, SIMD_8x32 &B6, SIMD_8x32 &B7)
 
static void zero_registers ()
 

Detailed Description

Definition at line 15 of file simd_avx2.h.

Constructor & Destructor Documentation

◆ SIMD_8x32() [1/6]

Botan::SIMD_8x32::SIMD_8x32 ( const SIMD_8x32 &  other)
default

◆ SIMD_8x32() [2/6]

Botan::SIMD_8x32::SIMD_8x32 ( SIMD_8x32 &&  other)
default

◆ SIMD_8x32() [3/6]

BOTAN_FORCE_INLINE Botan::SIMD_8x32::SIMD_8x32 ( )
inline

Definition at line 26 of file simd_avx2.h.

27 {
28 m_avx2 = _mm256_setzero_si256();
29 }

Referenced by andc(), BOTAN_FUNC_ISA(), bswap(), load_le(), operator~(), rotl(), and splat().

◆ SIMD_8x32() [4/6]

Botan::SIMD_8x32::SIMD_8x32 ( const uint32_t  B[8])
inlineexplicit

Definition at line 32 of file simd_avx2.h.

33 {
34 m_avx2 = _mm256_loadu_si256(reinterpret_cast<const __m256i*>(B));
35 }

◆ SIMD_8x32() [5/6]

Botan::SIMD_8x32::SIMD_8x32 ( uint32_t  B0,
uint32_t  B1,
uint32_t  B2,
uint32_t  B3,
uint32_t  B4,
uint32_t  B5,
uint32_t  B6,
uint32_t  B7 
)
inlineexplicit

Definition at line 38 of file simd_avx2.h.

40 {
41 m_avx2 = _mm256_set_epi32(B7, B6, B5, B4, B3, B2, B1, B0);
42 }

◆ SIMD_8x32() [6/6]

Botan::SIMD_8x32::SIMD_8x32 ( __m256i  x)
inline

Definition at line 281 of file simd_avx2.h.

281: m_avx2(x) {}

Member Function Documentation

◆ andc()

SIMD_8x32 Botan::SIMD_8x32::andc ( const SIMD_8x32 &  other) const
inline

Definition at line 212 of file simd_avx2.h.

213 {
214 return SIMD_8x32(_mm256_andnot_si256(m_avx2, other.m_avx2));
215 }
Botan::SIMD_8x32::SIMD_8x32
BOTAN_FORCE_INLINE SIMD_8x32()
Definition: simd_avx2.h:26

References SIMD_8x32().

◆ BOTAN_FUNC_ISA() [1/4]

__m256i Botan::SIMD_8x32::BOTAN_FUNC_ISA ( "avx2"  ) const
inline

Definition at line 278 of file simd_avx2.h.

278{ return m_avx2; }

◆ BOTAN_FUNC_ISA() [2/4]

template<size_t ROT1, size_t ROT2, size_t ROT3>
SIMD_8x32 Botan::SIMD_8x32::BOTAN_FUNC_ISA ( "avx2"  ) const
inline

Definition at line 113 of file simd_avx2.h.

114 {
115 SIMD_8x32 res;
116
117 const SIMD_8x32 rot1 = this->rotr<ROT1>();
118 const SIMD_8x32 rot2 = this->rotr<ROT2>();
119 const SIMD_8x32 rot3 = this->rotr<ROT3>();
120
121 return rot1 ^ rot2 ^ rot3;
122 }

◆ BOTAN_FUNC_ISA() [3/4]

template<int SHIFT>
Botan::SIMD_8x32::BOTAN_FUNC_ISA ( "avx2"  ) const
inline

Definition at line 194 of file simd_avx2.h.

195 {
196 return SIMD_8x32(_mm256_slli_epi32(m_avx2, SHIFT));
197 }

References SIMD_8x32().

◆ BOTAN_FUNC_ISA() [4/4]

template<int SHIFT>
Botan::SIMD_8x32::BOTAN_FUNC_ISA ( "avx2"  ) const
inline

Definition at line 199 of file simd_avx2.h.

200 {
201 return SIMD_8x32(_mm256_srli_epi32(m_avx2, SHIFT));
202 }

References SIMD_8x32().

◆ bswap()

SIMD_8x32 Botan::SIMD_8x32::bswap ( ) const
inline

Definition at line 218 of file simd_avx2.h.

219 {
220 const uint8_t BSWAP_MASK[32] = { 3, 2, 1, 0,
221 7, 6, 5, 4,
222 11, 10, 9, 8,
223 15, 14, 13, 12,
224 19, 18, 17, 16,
225 23, 22, 21, 20,
226 27, 26, 25, 24,
227 31, 30, 29, 28 };
228
229 const __m256i bswap = _mm256_loadu_si256(reinterpret_cast<const __m256i*>(BSWAP_MASK));
230
231 const __m256i output = _mm256_shuffle_epi8(m_avx2, bswap);
232
233 return SIMD_8x32(output);
234 }
Botan::SIMD_8x32::bswap
SIMD_8x32 bswap() const
Definition: simd_avx2.h:218

References bswap(), and SIMD_8x32().

Referenced by bswap(), load_be(), and store_be().

◆ load_be()

static SIMD_8x32 Botan::SIMD_8x32::load_be ( const uint8_t *  in)
inlinestatic

Definition at line 57 of file simd_avx2.h.

58 {
59 return load_le(in).bswap();
60 }
Botan::SIMD_8x32::load_le
static SIMD_8x32 load_le(const uint8_t *in)
Definition: simd_avx2.h:51

References bswap(), and load_le().

◆ load_le()

static SIMD_8x32 Botan::SIMD_8x32::load_le ( const uint8_t *  in)
inlinestatic

Definition at line 51 of file simd_avx2.h.

52 {
53 return SIMD_8x32(_mm256_loadu_si256(reinterpret_cast<const __m256i*>(in)));
54 }

References SIMD_8x32().

Referenced by load_be().

◆ operator&()

SIMD_8x32 Botan::SIMD_8x32::operator& ( const SIMD_8x32 &  other) const
inline

Definition at line 157 of file simd_avx2.h.

158 {
159 SIMD_8x32 retval(*this);
160 retval &= other;
161 return retval;
162 }

◆ operator&=()

void Botan::SIMD_8x32::operator&= ( const SIMD_8x32 &  other)
inline

Definition at line 189 of file simd_avx2.h.

190 {
191 m_avx2 = _mm256_and_si256(m_avx2, other.m_avx2);
192 }

◆ operator+()

SIMD_8x32 Botan::SIMD_8x32::operator+ ( const SIMD_8x32 &  other) const
inline

Definition at line 125 of file simd_avx2.h.

126 {
127 SIMD_8x32 retval(*this);
128 retval += other;
129 return retval;
130 }

◆ operator+=()

void Botan::SIMD_8x32::operator+= ( const SIMD_8x32 &  other)
inline

Definition at line 165 of file simd_avx2.h.

166 {
167 m_avx2 = _mm256_add_epi32(m_avx2, other.m_avx2);
168 }

◆ operator-()

SIMD_8x32 Botan::SIMD_8x32::operator- ( const SIMD_8x32 &  other) const
inline

Definition at line 133 of file simd_avx2.h.

134 {
135 SIMD_8x32 retval(*this);
136 retval -= other;
137 return retval;
138 }

◆ operator-=()

void Botan::SIMD_8x32::operator-= ( const SIMD_8x32 &  other)
inline

Definition at line 171 of file simd_avx2.h.

172 {
173 m_avx2 = _mm256_sub_epi32(m_avx2, other.m_avx2);
174 }

◆ operator=() [1/2]

SIMD_8x32 & Botan::SIMD_8x32::operator= ( const SIMD_8x32 &  other)
default

◆ operator=() [2/2]

SIMD_8x32 & Botan::SIMD_8x32::operator= ( SIMD_8x32 &&  other)
default

◆ operator^()

SIMD_8x32 Botan::SIMD_8x32::operator^ ( const SIMD_8x32 &  other) const
inline

Definition at line 141 of file simd_avx2.h.

142 {
143 SIMD_8x32 retval(*this);
144 retval ^= other;
145 return retval;
146 }

◆ operator^=()

void Botan::SIMD_8x32::operator^= ( const SIMD_8x32 &  other)
inline

Definition at line 177 of file simd_avx2.h.

178 {
179 m_avx2 = _mm256_xor_si256(m_avx2, other.m_avx2);
180 }

◆ operator|()

SIMD_8x32 Botan::SIMD_8x32::operator| ( const SIMD_8x32 &  other) const
inline

Definition at line 149 of file simd_avx2.h.

150 {
151 SIMD_8x32 retval(*this);
152 retval |= other;
153 return retval;
154 }

◆ operator|=()

void Botan::SIMD_8x32::operator|= ( const SIMD_8x32 &  other)
inline

Definition at line 183 of file simd_avx2.h.

184 {
185 m_avx2 = _mm256_or_si256(m_avx2, other.m_avx2);
186 }

◆ operator~()

SIMD_8x32 Botan::SIMD_8x32::operator~ ( ) const
inline

Definition at line 205 of file simd_avx2.h.

206 {
207 return SIMD_8x32(_mm256_xor_si256(m_avx2, _mm256_set1_epi32(0xFFFFFFFF)));
208 }

References SIMD_8x32().

◆ reset_registers()

static void Botan::SIMD_8x32::reset_registers ( )
inlinestatic

Definition at line 267 of file simd_avx2.h.

268 {
269 _mm256_zeroupper();
270 }

◆ rotl()

template<size_t ROT>
SIMD_8x32 Botan::SIMD_8x32::rotl ( ) const
inline

Definition at line 76 of file simd_avx2.h.

77 {
78 static_assert(ROT > 0 && ROT < 32, "Invalid rotation constant");
79
80#if defined(__AVX512VL__)
81 return SIMD_8x32(_mm256_rol_epi32(m_avx2, ROT));
82#else
83 BOTAN_IF_CONSTEXPR(ROT == 8)
84 {
85 const __m256i shuf_rotl_8 = _mm256_set_epi8(14, 13, 12, 15, 10, 9, 8, 11, 6, 5, 4, 7, 2, 1, 0, 3,
86 14, 13, 12, 15, 10, 9, 8, 11, 6, 5, 4, 7, 2, 1, 0, 3);
87
88 return SIMD_8x32(_mm256_shuffle_epi8(m_avx2, shuf_rotl_8));
89 }
90 else BOTAN_IF_CONSTEXPR(ROT == 16)
91 {
92 const __m256i shuf_rotl_16 = _mm256_set_epi8(13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2,
93 13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2);
94
95 return SIMD_8x32(_mm256_shuffle_epi8(m_avx2, shuf_rotl_16));
96 }
97 else
98 {
99 return SIMD_8x32(_mm256_or_si256(_mm256_slli_epi32(m_avx2, static_cast<int>(ROT)),
100 _mm256_srli_epi32(m_avx2, static_cast<int>(32-ROT))));
101 }
102#endif
103 }
BOTAN_IF_CONSTEXPR
#define BOTAN_IF_CONSTEXPR
Definition: compiler.h:176

References BOTAN_IF_CONSTEXPR, and SIMD_8x32().

Referenced by rotr().

◆ rotr()

template<size_t ROT>
SIMD_8x32 Botan::SIMD_8x32::rotr ( ) const
inline

Definition at line 107 of file simd_avx2.h.

108 {
109 return this->rotl<32-ROT>();
110 }
Botan::SIMD_8x32::rotl
SIMD_8x32 rotl() const
Definition: simd_avx2.h:76

References rotl().

◆ splat()

static SIMD_8x32 Botan::SIMD_8x32::splat ( uint32_t  B)
inlinestatic

Definition at line 45 of file simd_avx2.h.

46 {
47 return SIMD_8x32(_mm256_set1_epi32(B));
48 }

References SIMD_8x32().

◆ store_be()

void Botan::SIMD_8x32::store_be ( uint8_t  out[]) const
inline

Definition at line 69 of file simd_avx2.h.

70 {
71 bswap().store_le(out);
72 }
Botan::SIMD_8x32::store_le
void store_le(uint8_t out[]) const
Definition: simd_avx2.h:63

References bswap(), and store_le().

◆ store_le()

void Botan::SIMD_8x32::store_le ( uint8_t  out[]) const
inline

Definition at line 63 of file simd_avx2.h.

64 {
65 _mm256_storeu_si256(reinterpret_cast<__m256i*>(out), m_avx2);
66 }

Referenced by store_be().

◆ transpose() [1/2]

static void Botan::SIMD_8x32::transpose ( SIMD_8x32 &  B0,
SIMD_8x32 &  B1,
SIMD_8x32 &  B2,
SIMD_8x32 &  B3 
)
inlinestatic

Definition at line 237 of file simd_avx2.h.

239 {
240 const __m256i T0 = _mm256_unpacklo_epi32(B0.m_avx2, B1.m_avx2);
241 const __m256i T1 = _mm256_unpacklo_epi32(B2.m_avx2, B3.m_avx2);
242 const __m256i T2 = _mm256_unpackhi_epi32(B0.m_avx2, B1.m_avx2);
243 const __m256i T3 = _mm256_unpackhi_epi32(B2.m_avx2, B3.m_avx2);
244
245 B0.m_avx2 = _mm256_unpacklo_epi64(T0, T1);
246 B1.m_avx2 = _mm256_unpackhi_epi64(T0, T1);
247 B2.m_avx2 = _mm256_unpacklo_epi64(T2, T3);
248 B3.m_avx2 = _mm256_unpackhi_epi64(T2, T3);
249 }

Referenced by transpose().

◆ transpose() [2/2]

static void Botan::SIMD_8x32::transpose ( SIMD_8x32 &  B0,
SIMD_8x32 &  B1,
SIMD_8x32 &  B2,
SIMD_8x32 &  B3,
SIMD_8x32 &  B4,
SIMD_8x32 &  B5,
SIMD_8x32 &  B6,
SIMD_8x32 &  B7 
)
inlinestatic

Definition at line 252 of file simd_avx2.h.

256 {
257 transpose(B0, B1, B2, B3);
258 transpose(B4, B5, B6, B7);
259
260 swap_tops(B0, B4);
261 swap_tops(B1, B5);
262 swap_tops(B2, B6);
263 swap_tops(B3, B7);
264 }
Botan::SIMD_8x32::transpose
static void transpose(SIMD_8x32 &B0, SIMD_8x32 &B1, SIMD_8x32 &B2, SIMD_8x32 &B3)
Definition: simd_avx2.h:237

References transpose().

◆ zero_registers()

static void Botan::SIMD_8x32::zero_registers ( )
inlinestatic

Definition at line 273 of file simd_avx2.h.

274 {
275 _mm256_zeroall();
276 }
The documentation for this class was generated from the following file:
Generated by doxygen 1.9.3