Home
last modified time | relevance | path

Searched refs:ivreg (Results 1 – 2 of 2) sorted by relevance

/f-stack/freebsd/crypto/aesni/
H A Daesni_wrap.c60 __m128i tot, ivreg; in aesni_encrypt_cbc() local
64 ivreg = _mm_loadu_si128((const __m128i *)iv); in aesni_encrypt_cbc()
67 _mm_loadu_si128((const __m128i *)from) ^ ivreg); in aesni_encrypt_cbc()
68 ivreg = tot; in aesni_encrypt_cbc()
81 __m128i ivreg, nextiv; in aesni_decrypt_cbc() local
84 ivreg = _mm_loadu_si128((const __m128i *)iv); in aesni_decrypt_cbc()
93 blks->blk[j] = blocks[j] ^ ivreg; in aesni_decrypt_cbc()
94 ivreg = nextiv; in aesni_decrypt_cbc()
103 aesni_dec(rounds - 1, key_schedule, nextiv) ^ ivreg); in aesni_decrypt_cbc()
104 ivreg = nextiv; in aesni_decrypt_cbc()
/f-stack/freebsd/crypto/armv8/
H A Darmv8_crypto_wrap.c99 uint8x16_t tot, ivreg, tmp; in armv8_aes_encrypt_cbc() local
103 ivreg = vld1q_u8(iv); in armv8_aes_encrypt_cbc()
107 (const void*)key->aes_key, veorq_u8(tmp, ivreg)); in armv8_aes_encrypt_cbc()
108 ivreg = tot; in armv8_aes_encrypt_cbc()
119 uint8x16_t ivreg, nextiv, tmp; in armv8_aes_decrypt_cbc() local
123 ivreg = vld1q_u8(iv); in armv8_aes_decrypt_cbc()
128 vst1q_u8(buf, veorq_u8(tmp, ivreg)); in armv8_aes_decrypt_cbc()
129 ivreg = nextiv; in armv8_aes_decrypt_cbc()