/freebsd/contrib/bearssl/src/symcipher/ |
H A D | chacha20_sse2.c | 190 _mm_storeu_si128((void *)(tmp + 0), s0); in br_chacha20_sse2_run() 191 _mm_storeu_si128((void *)(tmp + 16), s1); in br_chacha20_sse2_run() 192 _mm_storeu_si128((void *)(tmp + 32), s2); in br_chacha20_sse2_run() 193 _mm_storeu_si128((void *)(tmp + 48), s3); in br_chacha20_sse2_run() 209 _mm_storeu_si128((void *)(buf + 0), b0); in br_chacha20_sse2_run() 210 _mm_storeu_si128((void *)(buf + 16), b1); in br_chacha20_sse2_run() 211 _mm_storeu_si128((void *)(buf + 32), b2); in br_chacha20_sse2_run() 212 _mm_storeu_si128((void *)(buf + 48), b3); in br_chacha20_sse2_run()
|
H A D | aes_x86ni_ctrcbc.c | 192 _mm_storeu_si128((void *)(buf + 0), x0); in br_aes_x86ni_ctrcbc_ctr() 193 _mm_storeu_si128((void *)(buf + 16), x1); in br_aes_x86ni_ctrcbc_ctr() 194 _mm_storeu_si128((void *)(buf + 32), x2); in br_aes_x86ni_ctrcbc_ctr() 195 _mm_storeu_si128((void *)(buf + 48), x3); in br_aes_x86ni_ctrcbc_ctr() 201 _mm_storeu_si128((void *)(tmp + 0), x0); in br_aes_x86ni_ctrcbc_ctr() 202 _mm_storeu_si128((void *)(tmp + 16), x1); in br_aes_x86ni_ctrcbc_ctr() 302 _mm_storeu_si128(cbcmac, ivx); in br_aes_x86ni_ctrcbc_mac() 403 _mm_storeu_si128((void *)buf, x0); in br_aes_x86ni_ctrcbc_encrypt() 451 _mm_storeu_si128(cbcmac, cmx); in br_aes_x86ni_ctrcbc_encrypt() 544 _mm_storeu_si128((void *)buf, x0); in br_aes_x86ni_ctrcbc_decrypt() [all …]
|
H A D | aes_x86ni_ctr.c | 164 _mm_storeu_si128((void *)(buf + 0), x0); in br_aes_x86ni_ctr_run() 165 _mm_storeu_si128((void *)(buf + 16), x1); in br_aes_x86ni_ctr_run() 166 _mm_storeu_si128((void *)(buf + 32), x2); in br_aes_x86ni_ctr_run() 167 _mm_storeu_si128((void *)(buf + 48), x3); in br_aes_x86ni_ctr_run() 174 _mm_storeu_si128((void *)(tmp + 0), x0); in br_aes_x86ni_ctr_run() 175 _mm_storeu_si128((void *)(tmp + 16), x1); in br_aes_x86ni_ctr_run() 176 _mm_storeu_si128((void *)(tmp + 32), x2); in br_aes_x86ni_ctr_run() 177 _mm_storeu_si128((void *)(tmp + 48), x3); in br_aes_x86ni_ctr_run()
|
H A D | aes_x86ni_cbcdec.c | 180 _mm_storeu_si128((void *)(buf + 0), x0); in br_aes_x86ni_cbcdec_run() 182 _mm_storeu_si128((void *)(buf + 16), x1); in br_aes_x86ni_cbcdec_run() 183 _mm_storeu_si128((void *)(buf + 32), x2); in br_aes_x86ni_cbcdec_run() 184 _mm_storeu_si128((void *)(buf + 48), x3); in br_aes_x86ni_cbcdec_run() 189 _mm_storeu_si128((void *)(buf + 16), x1); in br_aes_x86ni_cbcdec_run() 191 _mm_storeu_si128( in br_aes_x86ni_cbcdec_run() 198 _mm_storeu_si128(iv, ivx); in br_aes_x86ni_cbcdec_run()
|
H A D | aes_x86ni_cbcenc.c | 93 _mm_storeu_si128((void *)buf, x); in br_aes_x86ni_cbcenc_run() 97 _mm_storeu_si128(iv, ivx); in br_aes_x86ni_cbcenc_run()
|
H A D | aes_x86ni.c | 229 _mm_storeu_si128((void *)skni, sk[num_rounds]); in br_aes_x86ni_keysched_dec() 231 _mm_storeu_si128((void *)(skni + (u << 4)), in br_aes_x86ni_keysched_dec() 234 _mm_storeu_si128((void *)(skni + (num_rounds << 4)), sk[0]); in br_aes_x86ni_keysched_dec()
|
/freebsd/sys/crypto/aesni/ |
H A D | aesni_wrap.c | 66 _mm_storeu_si128((__m128i *)to, tot); in aesni_encrypt_cbc() 99 _mm_storeu_si128((void *)buf, in aesni_decrypt_cbc() 139 _mm_storeu_si128((__m128i *)to, tot); in aesni_encrypt_ecb() 178 _mm_storeu_si128((__m128i *)to, tot); in aesni_decrypt_ecb() 268 _mm_storeu_si128((__m128i *)to, tot); in aesni_encrypt_icm() 373 _mm_storeu_si128(&top[0], tmp[0] ^ tweaks[0]); in aesni_crypt_xts_block8() 374 _mm_storeu_si128(&top[1], tmp[1] ^ tweaks[1]); in aesni_crypt_xts_block8() 375 _mm_storeu_si128(&top[2], tmp[2] ^ tweaks[2]); in aesni_crypt_xts_block8() 376 _mm_storeu_si128(&top[3], tmp[3] ^ tweaks[3]); in aesni_crypt_xts_block8() 377 _mm_storeu_si128(&top[4], tmp[4] ^ tweaks[4]); in aesni_crypt_xts_block8() [all …]
|
H A D | aesni_ghash.c | 453 _mm_storeu_si128(&((__m128i*)out)[i*8+0], tmp1); in AES_GCM_encrypt() 454 _mm_storeu_si128(&((__m128i*)out)[i*8+1], tmp2); in AES_GCM_encrypt() 455 _mm_storeu_si128(&((__m128i*)out)[i*8+2], tmp3); in AES_GCM_encrypt() 456 _mm_storeu_si128(&((__m128i*)out)[i*8+3], tmp4); in AES_GCM_encrypt() 457 _mm_storeu_si128(&((__m128i*)out)[i*8+4], tmp5); in AES_GCM_encrypt() 458 _mm_storeu_si128(&((__m128i*)out)[i*8+5], tmp6); in AES_GCM_encrypt() 459 _mm_storeu_si128(&((__m128i*)out)[i*8+6], tmp7); in AES_GCM_encrypt() 460 _mm_storeu_si128(&((__m128i*)out)[i*8+7], tmp8); in AES_GCM_encrypt() 490 _mm_storeu_si128(&((__m128i*)out)[k], tmp1); in AES_GCM_encrypt() 525 _mm_storeu_si128((__m128i*)tag, T); in AES_GCM_encrypt() [all …]
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_stream/chacha20/dolbeau/ |
H A D | u0.h | 76 _mm_storeu_si128((__m128i*) (partialblock + 0), x_0); 77 _mm_storeu_si128((__m128i*) (partialblock + 16), x_1); 78 _mm_storeu_si128((__m128i*) (partialblock + 32), x_2); 79 _mm_storeu_si128((__m128i*) (partialblock + 48), x_3);
|
H A D | u1.h | 81 _mm_storeu_si128((__m128i*) (c + 0), x_0); 82 _mm_storeu_si128((__m128i*) (c + 16), x_1); 83 _mm_storeu_si128((__m128i*) (c + 32), x_2); 84 _mm_storeu_si128((__m128i*) (c + 48), x_3);
|
H A D | u4.h | 141 _mm_storeu_si128((__m128i*) (c + 0), t0); \ 143 _mm_storeu_si128((__m128i*) (c + 64), t1); \ 145 _mm_storeu_si128((__m128i*) (c + 128), t2); \ 147 _mm_storeu_si128((__m128i*) (c + 192), t3); \
|
H A D | u8.h | 248 _mm_storeu_si128((__m128i*) (c + 0), t0); \ 251 _mm_storeu_si128((__m128i*) (c + 64), t1); \ 254 _mm_storeu_si128((__m128i*) (c + 128), t2); \ 257 _mm_storeu_si128((__m128i*) (c + 192), t3); \ 260 _mm_storeu_si128((__m128i*) (c + 256), t0); \ 263 _mm_storeu_si128((__m128i*) (c + 320), t1); \ 266 _mm_storeu_si128((__m128i*) (c + 384), t2); \ 269 _mm_storeu_si128((__m128i*) (c + 448), t3); \
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_onetimeauth/poly1305/sse2/ |
H A D | poly1305_sse2.c | 117 _mm_storeu_si128((xmmi *) (void *) &st->H.hh[0], _mm_setzero_si128()); in poly1305_init_ext() 681 _mm_storeu_si128((xmmi *) (void *) &st->H.hh[0], T0); in poly1305_blocks() 682 _mm_storeu_si128((xmmi *) (void *) &st->H.hh[4], T1); in poly1305_blocks() 854 _mm_storeu_si128((xmmi *) (void *) st + 0, _mm_setzero_si128()); in poly1305_finish_ext() 855 _mm_storeu_si128((xmmi *) (void *) st + 1, _mm_setzero_si128()); in poly1305_finish_ext() 856 _mm_storeu_si128((xmmi *) (void *) st + 2, _mm_setzero_si128()); in poly1305_finish_ext() 857 _mm_storeu_si128((xmmi *) (void *) st + 3, _mm_setzero_si128()); in poly1305_finish_ext() 858 _mm_storeu_si128((xmmi *) (void *) st + 4, _mm_setzero_si128()); in poly1305_finish_ext() 859 _mm_storeu_si128((xmmi *) (void *) st + 5, _mm_setzero_si128()); in poly1305_finish_ext() 860 _mm_storeu_si128((xmmi *) (void *) st + 6, _mm_setzero_si128()); in poly1305_finish_ext() [all …]
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_stream/salsa20/xmm6int/ |
H A D | u8.h | 381 _mm_storeu_si128((__m128i*) (c + 0), t0); \ 384 _mm_storeu_si128((__m128i*) (c + 64), t1); \ 387 _mm_storeu_si128((__m128i*) (c + 128), t2); \ 390 _mm_storeu_si128((__m128i*) (c + 192), t3); \ 393 _mm_storeu_si128((__m128i*) (c + 256), t0); \ 396 _mm_storeu_si128((__m128i*) (c + 320), t1); \ 399 _mm_storeu_si128((__m128i*) (c + 384), t2); \ 402 _mm_storeu_si128((__m128i*) (c + 448), t3); \
|
H A D | u4.h | 515 _mm_storeu_si128((__m128i *) (c + 0), y##A); \ 517 _mm_storeu_si128((__m128i *) (c + 64), y##B); \ 519 _mm_storeu_si128((__m128i *) (c + 128), y##C); \ 521 _mm_storeu_si128((__m128i *) (c + 192), y##D)
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_pwhash/argon2/ |
H A D | argon2-fill-block-ssse3.c | 63 _mm_storeu_si128((__m128i *) (&next_block[16 * i]), state[i]); in fill_block() 95 _mm_storeu_si128((__m128i *) (&next_block[16 * i]), state[i]); in fill_block_with_xor()
|
/freebsd/sys/contrib/libb2/ |
H A D | blake2s-round.h | 21 #define STOREU(p,r) _mm_storeu_si128((__m128i *)(p), r)
|
H A D | blake2b-round.h | 21 #define STOREU(p,r) _mm_storeu_si128((__m128i *)(p), r)
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/ |
H A D | blake2b-compress-sse41.h | 6 #define STOREU(p, r) _mm_storeu_si128((__m128i *) (void *) (p), r)
|
H A D | blake2b-compress-ssse3.h | 6 #define STOREU(p, r) _mm_storeu_si128((__m128i *) (void *) (p), r)
|
H A D | blake2b-compress-avx2.h | 6 #define STOREU128(p, r) _mm_storeu_si128((__m128i *) (p), r)
|
/freebsd/sys/contrib/zstd/lib/common/ |
H A D | zstd_internal.h | 189 _mm_storeu_si128((__m128i*)dst, _mm_loadu_si128((const __m128i*)src)); in ZSTD_copy16()
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_aead/aes256gcm/aesni/ |
H A D | aead_aes256gcm_aesni.c | 120 _mm_storeu_si128((__m128i *) out, temp); in aesni_encrypt1() 154 _mm_storeu_si128((__m128i *) (out + (a * 16)), temp##a) 261 _mm_storeu_si128((__m128i *) c, tmp21); in addmul()
|
/freebsd/contrib/bearssl/src/hash/ |
H A D | ghash_pclmul.c | 375 _mm_storeu_si128(y, yw); in br_ghash_pclmul()
|
/freebsd/contrib/llvm-project/clang/lib/Headers/ |
H A D | avxintrin.h | 5104 _mm_storeu_si128(__addr_lo, __v128); in _mm256_storeu2_m128i() 5106 _mm_storeu_si128(__addr_hi, __v128); in _mm256_storeu2_m128i()
|