Home
last modified time | relevance | path

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

/src/sys/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()
53 const __m128i m5 = LOADU(block + 80); in blake2b_compress_sse41()
54 const __m128i m6 = LOADU(block + 96); in blake2b_compress_sse41()
55 const __m128i m7 = LOADU(block + 112); in blake2b_compress_sse41()
56 row1l = LOADU(&S->h[0]); in blake2b_compress_sse41()
57 row1h = LOADU(&S->h[2]); 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
/src/sys/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()
303 const __m128i m3 = LOADU( block + 48 ); in blake2b_compress()
304 const __m128i m4 = LOADU( block + 64 ); in blake2b_compress()
305 const __m128i m5 = LOADU( block + 80 ); in blake2b_compress()
306 const __m128i m6 = LOADU( block + 96 ); in blake2b_compress()
307 const __m128i m7 = LOADU( block + 112 ); in blake2b_compress()
326 row1l = LOADU( &S->h[0] ); in blake2b_compress()
327 row1h = LOADU( &S->h[2] ); 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