/netbsd-src/sys/crypto/chacha/ |
H A D | chacha_ref.c | 71 uint32_t y0,y1,y2,y3,y4,y5,y6,y7,y8,y9,y10,y11,y12,y13,y14,y15; in chacha_core_ref() local 83 x10 = y10 = le32dec(k + 24); in chacha_core_ref() 93 CHACHA_QUARTERROUND( y2, y6,y10,y14); in chacha_core_ref() 95 CHACHA_QUARTERROUND( y0, y5,y10,y15); in chacha_core_ref() 111 le32enc(out + 40, x10 + y10); in chacha_core_ref() 130 uint32_t y0,y1,y2,y3,y4,y5,y6,y7,y8,y9,y10,y11,y12,y13,y14,y15; in chacha_stream_ref() local 161 y10 = x10; in chacha_stream_ref() 170 CHACHA_QUARTERROUND( y2, y6,y10,y14); in chacha_stream_ref() 172 CHACHA_QUARTERROUND( y0, y5,y10,y15); in chacha_stream_ref() 187 le32enc(s + 40, x10 + y10); in chacha_stream_ref() [all …]
|
/netbsd-src/sys/crypto/chacha/arch/x86/ |
H A D | chacha_sse2.c | 200 __m128i y0,y1,y2,y3,y4,y5,y6,y7,y8,y9,y10,y11,y12,y13,y14,y15; in chacha_stream_sse2() local 237 y10 = x10; in chacha_stream_sse2() 246 CHACHA_QUARTERROUND( y2, y6,y10,y14); in chacha_stream_sse2() 248 CHACHA_QUARTERROUND( y0, y5,y10,y15); in chacha_stream_sse2() 263 y10 = _mm_add_epi32(y10, x10); in chacha_stream_sse2() 272 z2 = unpack0_epi32(y8, y9, y10, y11); in chacha_stream_sse2() 276 z6 = unpack1_epi32(y8, y9, y10, y11); in chacha_stream_sse2() 280 z10 = unpack2_epi32(y8, y9, y10, y11); in chacha_stream_sse2() 284 z14 = unpack3_epi32(y8, y9, y10, y11); in chacha_stream_sse2() 356 __m128i y0,y1,y2,y3,y4,y5,y6,y7,y8,y9,y10,y11,y12,y13,y14,y15; in chacha_stream_xor_sse2() local [all …]
|
/netbsd-src/sys/external/isc/libsodium/dist/src/libsodium/crypto_stream/salsa20/xmm6int/ |
H A D | u8.h | 2 __m256i y0, y1, y2, y3, y4, y5, y6, y7, y8, y9, y10, y11, y12, y13, y14, variable 217 y10 = z2; 218 y10 = _mm256_add_epi32(y10, z6); 219 r10 = y10; 220 y10 = _mm256_slli_epi32(y10, 18); 221 z10 = _mm256_xor_si256(z10, y10); 345 y10 = z8; 346 y10 = _mm256_add_epi32(y10, z9); 347 r10 = y10; 348 y10 = _mm256_slli_epi32(y10, 18); [all …]
|
H A D | u4.h | 2 __m128i y0, y1, y2, y3, y4, y5, y6, y7, y8, y9, y10, y11, y12, y13, y14, variable 217 y10 = z2; 218 y10 = _mm_add_epi32(y10, z6); 219 r10 = y10; 220 y10 = _mm_slli_epi32(y10, 18); 221 z10 = _mm_xor_si128(z10, y10); 345 y10 = z8; 346 y10 = _mm_add_epi32(y10, z9); 347 r10 = y10; 348 y10 = _mm_slli_epi32(y10, 18); [all …]
|
/netbsd-src/sys/crypto/aes/ |
H A D | aes_ct.c | 56 uint32_t y10, y11, y12, y13, y14, y15, y16, y17, y18, y19; in br_aes_ct_bitslice_Sbox() local 96 y10 = y15 ^ t0; in br_aes_ct_bitslice_Sbox() 99 y17 = y10 ^ y11; in br_aes_ct_bitslice_Sbox() 100 y19 = y10 ^ y8; in br_aes_ct_bitslice_Sbox() 121 t15 = y8 & y10; in br_aes_ct_bitslice_Sbox() 162 z8 = t41 & y10; in br_aes_ct_bitslice_Sbox()
|
/netbsd-src/sys/crypto/aes/arch/x86/ |
H A D | aes_sse2.c | 59 __m128i y10, y11, y12, y13, y14, y15, y16, y17, y18, y19; in aes_sse2_bitslice_Sbox() local 99 y10 = y15 ^ t0; in aes_sse2_bitslice_Sbox() 102 y17 = y10 ^ y11; in aes_sse2_bitslice_Sbox() 103 y19 = y10 ^ y8; in aes_sse2_bitslice_Sbox() 124 t15 = y8 & y10; in aes_sse2_bitslice_Sbox() 165 z8 = t41 & y10; in aes_sse2_bitslice_Sbox()
|