Searched refs:ivreg (Results 1 – 2 of 2) sorted by relevance
| /freebsd/sys/crypto/armv8/ |
| H A D | armv8_crypto_wrap.c | 104 uint8x16_t tot, ivreg, tmp; in armv8_aes_encrypt_cbc() local
111 ivreg = vld1q_u8(iv); in armv8_aes_encrypt_cbc()
121 (const void *)key->aes_key, veorq_u8(tmp, ivreg)); in armv8_aes_encrypt_cbc()
122 ivreg = tot; in armv8_aes_encrypt_cbc()
132 veorq_u8(tmp, ivreg)); in armv8_aes_encrypt_cbc()
133 ivreg = tot; in armv8_aes_encrypt_cbc()
152 uint8x16_t ivreg, nextiv, tmp; in armv8_aes_decrypt_cbc() local
159 ivreg = vld1q_u8(iv); in armv8_aes_decrypt_cbc()
170 vst1q_u8(block, veorq_u8(tmp, ivreg)); in armv8_aes_decrypt_cbc()
171 ivreg = nextiv; in armv8_aes_decrypt_cbc()
[all …]
|
| /freebsd/sys/crypto/aesni/ |
| H A D | aesni_wrap.c | 57 __m128i tot, ivreg; in aesni_encrypt_cbc() local
61 ivreg = _mm_loadu_si128((const __m128i *)iv); in aesni_encrypt_cbc()
64 _mm_loadu_si128((const __m128i *)from) ^ ivreg); in aesni_encrypt_cbc()
65 ivreg = tot; in aesni_encrypt_cbc()
78 __m128i ivreg, nextiv; in aesni_decrypt_cbc() local
81 ivreg = _mm_loadu_si128((const __m128i *)iv); in aesni_decrypt_cbc()
90 blks->blk[j] = blocks[j] ^ ivreg; in aesni_decrypt_cbc()
91 ivreg = nextiv; in aesni_decrypt_cbc()
100 aesni_dec(rounds - 1, key_schedule, nextiv) ^ ivreg); in aesni_decrypt_cbc()
101 ivreg = nextiv; in aesni_decrypt_cbc()
|