Home
last modified time | relevance | path

Searched refs:LOADU (Results 1 – 10 of 10) sorted by relevance

/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-sse41.c48 const __m128i m0 = LOADU(block + 00); in blake2b_compress_sse41()
49 const __m128i m1 = LOADU(block + 16); in blake2b_compress_sse41()
50 const __m128i m2 = LOADU(block + 32); in blake2b_compress_sse41()
51 const __m128i m3 = LOADU(block + 48); in blake2b_compress_sse41()
52 const __m128i m4 = LOADU(block + 64); in blake2b_compress_sse41()
56 row1l = LOADU(&S->h[0]); in blake2b_compress_sse41()
57 row1h = LOADU(&S->h[2]); in blake2b_compress_sse41()
58 row2l = LOADU(&S->h[4]); in blake2b_compress_sse41()
59 row2h = LOADU(&S->h[6]); in blake2b_compress_sse41()
62 row4l = _mm_xor_si128(LOADU(&blake2b_IV[4]), LOADU(&S->t[0])); in blake2b_compress_sse41()
[all …]
H A Dblake2b-compress-ssse3.c59 row1l = LOADU(&S->h[0]); in blake2b_compress_ssse3()
60 row1h = LOADU(&S->h[2]); in blake2b_compress_ssse3()
61 row2l = LOADU(&S->h[4]); in blake2b_compress_ssse3()
62 row2h = LOADU(&S->h[6]); in blake2b_compress_ssse3()
63 row3l = LOADU(&blake2b_IV[0]); in blake2b_compress_ssse3()
64 row3h = LOADU(&blake2b_IV[2]); in blake2b_compress_ssse3()
65 row4l = _mm_xor_si128(LOADU(&blake2b_IV[4]), LOADU(&S->t[0])); in blake2b_compress_ssse3()
66 row4h = _mm_xor_si128(LOADU(&blake2b_IV[6]), LOADU(&S->f[0])); in blake2b_compress_ssse3()
81 STOREU(&S->h[0], _mm_xor_si128(LOADU(&S->h[0]), row1l)); in blake2b_compress_ssse3()
82 STOREU(&S->h[2], _mm_xor_si128(LOADU(&S->h[2]), row1h)); in blake2b_compress_ssse3()
[all …]
H A Dblake2b-compress-avx2.c40 __m256i a = LOADU(&S->h[0]); in blake2b_compress_avx2()
41 __m256i b = LOADU(&S->h[4]); in blake2b_compress_avx2()
H A Dblake2b-compress-sse41.h5 #define LOADU(p) _mm_loadu_si128((const __m128i *) (const void *) (p)) macro
H A Dblake2b-compress-ssse3.h5 #define LOADU(p) _mm_loadu_si128((const __m128i *) (const void *) (p)) macro
H A Dblake2b-compress-avx2.h11 #define LOADU(p) _mm256_loadu_si256((__m256i *) (p)) macro
/f-stack/freebsd/contrib/libb2/
H A Dblake2b.c300 const __m128i m0 = LOADU( block + 00 ); in blake2b_compress()
301 const __m128i m1 = LOADU( block + 16 ); in blake2b_compress()
302 const __m128i m2 = LOADU( block + 32 ); in blake2b_compress()
326 row1l = LOADU( &S->h[0] ); in blake2b_compress()
327 row1h = LOADU( &S->h[2] ); in blake2b_compress()
328 row2l = LOADU( &S->h[4] ); in blake2b_compress()
329 row2h = LOADU( &S->h[6] ); in blake2b_compress()
330 row3l = LOADU( &blake2b_IV[0] ); in blake2b_compress()
331 row3h = LOADU( &blake2b_IV[2] ); in blake2b_compress()
332 row4l = _mm_xor_si128( LOADU( &blake2b_IV[4] ), LOADU( &S->t[0] ) ); in blake2b_compress()
[all …]
H A Dblake2s.c289 const __m128i m0 = LOADU( block + 00 ); in blake2s_compress()
290 const __m128i m1 = LOADU( block + 16 ); in blake2s_compress()
291 const __m128i m2 = LOADU( block + 32 ); in blake2s_compress()
292 const __m128i m3 = LOADU( block + 48 ); in blake2s_compress()
311 row1 = ff0 = LOADU( &S->h[0] ); in blake2s_compress()
312 row2 = ff1 = LOADU( &S->h[4] ); in blake2s_compress()
314 …row4 = _mm_xor_si128( _mm_setr_epi32( 0x510E527F, 0x9B05688C, 0x1F83D9AB, 0x5BE0CD19 ), LOADU( &S-… in blake2s_compress()
H A Dblake2s-round.h20 #define LOADU(p) _mm_loadu_si128( (__m128i *)(p) ) macro
H A Dblake2b-round.h20 #define LOADU(p) _mm_loadu_si128( (__m128i *)(p) ) macro