| /f-stack/freebsd/opencrypto/ |
| H A D | xform_aes_xts.c | 92 ctx->tweak[i] = blocknum & 0xff; in aes_xts_reinit()
96 bzero(ctx->tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in aes_xts_reinit()
98 rijndael_encrypt(&ctx->key2, ctx->tweak, ctx->tweak); in aes_xts_reinit()
109 block[i] = in[i] ^ ctx->tweak[i]; in aes_xts_crypt()
117 out[i] ^= ctx->tweak[i]; in aes_xts_crypt()
122 carry_out = ctx->tweak[i] & 0x80; in aes_xts_crypt()
123 ctx->tweak[i] = (ctx->tweak[i] << 1) | (carry_in ? 1 : 0); in aes_xts_crypt()
127 ctx->tweak[0] ^= AES_XTS_ALPHA; in aes_xts_crypt()
|
| H A D | xform_enc.h | 96 uint8_t tweak[AES_XTS_BLOCKSIZE]; member
|
| /f-stack/freebsd/crypto/aesni/ |
| H A D | aesni_wrap.c | 308 aesni_crypt_xts_block(int rounds, const __m128i *key_schedule, __m128i *tweak, in aesni_crypt_xts_block() argument
313 block = _mm_loadu_si128((const __m128i *)from) ^ *tweak; in aesni_crypt_xts_block()
320 _mm_storeu_si128((__m128i *)to, block ^ *tweak); in aesni_crypt_xts_block()
322 *tweak = xts_crank_lfsr(*tweak); in aesni_crypt_xts_block()
326 aesni_crypt_xts_block8(int rounds, const __m128i *key_schedule, __m128i *tweak, in aesni_crypt_xts_block8() argument
336 tmptweak = *tweak; in aesni_crypt_xts_block8()
358 *tweak = tmptweak; in aesni_crypt_xts_block8()
384 uint8_t tweak[AES_XTS_BLOCKSIZE] __aligned(16); in aesni_crypt_xts() local
392 bcopy(iv, tweak, AES_XTS_IVSIZE); in aesni_crypt_xts()
394 bzero(tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in aesni_crypt_xts()
[all …]
|
| /f-stack/freebsd/crypto/armv8/ |
| H A D | armv8_crypto_wrap.c | 158 uint8x16_t *tweak, const uint8_t *from, uint8_t *to, int do_encrypt) in armv8_aes_crypt_xts_block() argument
162 block = vld1q_u8(from) ^ *tweak; in armv8_aes_crypt_xts_block()
169 vst1q_u8(to, block ^ *tweak); in armv8_aes_crypt_xts_block()
171 *tweak = vreinterpretq_u8_s32(xts_crank_lfsr(vreinterpretq_s32_u8(*tweak))); in armv8_aes_crypt_xts_block()
180 uint8_t tweak[AES_XTS_BLOCKSIZE] __aligned(16); in armv8_aes_crypt_xts() local
188 bcopy(iv, tweak, AES_XTS_IVSIZE); in armv8_aes_crypt_xts()
190 bzero(tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in armv8_aes_crypt_xts()
194 tweakreg = vld1q_u8(tweak); in armv8_aes_crypt_xts()
|
| /f-stack/freebsd/crypto/openssl/arm/ |
| H A D | bsaes-armv7.S | 1588 ldr r0, [ip] @ pointer to input tweak
1590 @ generate initial tweak
1604 sub r12, #48 @ place for tweak[9]
1628 sub sp, #0x90 @ place for tweak[9]
1631 vld1.8 {q8}, [r0] @ initial tweak
1995 vmov q8, q9 @ next round tweak
2070 @ generate initial tweak
2084 sub r12, #48 @ place for tweak[9]
2114 sub sp, #0x90 @ place for tweak[9]
2116 vld1.8 {q8}, [r0] @ initial tweak
[all …]
|
| /f-stack/freebsd/crypto/skein/amd64/ |
| H A D | skein_block_asm.s | 95 TWEAK = 8 + BCNT #tweak values[0..1]
278 StackVar ksTwk ,8*3 #key schedule: tweak words
297 StackVar bitAdd ,8 #bit count to add to tweak
|
| /f-stack/freebsd/contrib/device-tree/Bindings/memory-controllers/ |
| H A D | ti-da8xx-ddrctl.txt | 4 a set of registers which allow to tweak the controller's behavior.
|
| /f-stack/freebsd/contrib/device-tree/Bindings/soc/qcom/ |
| H A D | qcom,glink.txt | 57 to tweak the default intents available for the channel to
|
| /f-stack/freebsd/contrib/device-tree/src/arm/ |
| H A D | sun8i-h3-nanopi-duo2.dts | 3 * Copyright (C) 2019 Karl Palsson <karlp@tweak.net.au>
|
| H A D | armada-xp-lenovo-ix4-300d.dts | 228 * them up does the tweak) for poweroff to shutdown otherwise it
|
| /f-stack/freebsd/contrib/device-tree/Bindings/sound/ |
| H A D | cs42l42.txt | 76 hardware setups, a designer might want to tweak this. This is an array of
|
| /f-stack/app/redis-5.0.5/deps/jemalloc/ |
| H A D | ChangeLog | 697 --with-lg-tiny-min options, which can be used to tweak page and size class
|
| /f-stack/app/redis-5.0.5/ |
| H A D | 00-RELEASENOTES | 696 tweak form feedback
|
| /f-stack/freebsd/contrib/dev/acpica/ |
| H A D | changes.txt | 16669 load. This was a relatively minor tweak to the table loading code
|