Home
last modified time | relevance | path

Searched refs:_mm_storeu_si128 (Results 1 – 25 of 30) sorted by relevance

12

/freebsd/contrib/bearssl/src/symcipher/
H A Dchacha20_sse2.c190 _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 Daes_x86ni_ctrcbc.c192 _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 Daes_x86ni_ctr.c164 _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 Daes_x86ni_cbcdec.c180 _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 Daes_x86ni_cbcenc.c93 _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 Daes_x86ni.c229 _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 Daesni_wrap.c66 _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 Daesni_ghash.c453 _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 Du0.h76 _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 Du1.h81 _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 Du4.h141 _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 Du8.h248 _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 Dpoly1305_sse2.c117 _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 Du8.h381 _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 Du4.h515 _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 Dargon2-fill-block-ssse3.c63 _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 Dblake2s-round.h21 #define STOREU(p,r) _mm_storeu_si128((__m128i *)(p), r)
H A Dblake2b-round.h21 #define STOREU(p,r) _mm_storeu_si128((__m128i *)(p), r)
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-sse41.h6 #define STOREU(p, r) _mm_storeu_si128((__m128i *) (void *) (p), r)
H A Dblake2b-compress-ssse3.h6 #define STOREU(p, r) _mm_storeu_si128((__m128i *) (void *) (p), r)
H A Dblake2b-compress-avx2.h6 #define STOREU128(p, r) _mm_storeu_si128((__m128i *) (p), r)
/freebsd/sys/contrib/zstd/lib/common/
H A Dzstd_internal.h189 _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 Daead_aes256gcm_aesni.c120 _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 Dghash_pclmul.c375 _mm_storeu_si128(y, yw); in br_ghash_pclmul()
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A Davxintrin.h5104 _mm_storeu_si128(__addr_lo, __v128); in _mm256_storeu2_m128i()
5106 _mm_storeu_si128(__addr_hi, __v128); in _mm256_storeu2_m128i()

12