Home
last modified time | relevance | path

Searched refs:tweak (Results 1 – 25 of 70) sorted by relevance

123

/freebsd/crypto/openssl/crypto/modes/
H A Dxts128.c33 } tweak, scratch; in CRYPTO_xts128_encrypt() local
39 memcpy(tweak.c, iv, 16); in CRYPTO_xts128_encrypt()
41 (*ctx->block2)(tweak.c, tweak.c, ctx->key2); in CRYPTO_xts128_encrypt()
49 scratch.u[0] ^= tweak.u[0]; in CRYPTO_xts128_encrypt()
50 scratch.u[1] ^= tweak.u[1]; in CRYPTO_xts128_encrypt()
52 scratch.u[0] = ((u64_a1 *)inp)[0] ^ tweak.u[0]; in CRYPTO_xts128_encrypt()
53 scratch.u[1] = ((u64_a1 *)inp)[1] ^ tweak.u[1]; in CRYPTO_xts128_encrypt()
57 scratch.u[0] ^= tweak.u[0]; in CRYPTO_xts128_encrypt()
58 scratch.u[1] ^= tweak.u[1]; in CRYPTO_xts128_encrypt()
61 ((u64_a1 *)out)[0] = scratch.u[0] ^= tweak.u[0]; in CRYPTO_xts128_encrypt()
[all …]
H A Dxts128gb.c33 } tweak, scratch; in ossl_crypto_xts128gb_encrypt() local
39 memcpy(tweak.c, iv, 16); in ossl_crypto_xts128gb_encrypt()
41 (*ctx->block2)(tweak.c, tweak.c, ctx->key2); in ossl_crypto_xts128gb_encrypt()
49 scratch.u[0] ^= tweak.u[0]; in ossl_crypto_xts128gb_encrypt()
50 scratch.u[1] ^= tweak.u[1]; in ossl_crypto_xts128gb_encrypt()
52 scratch.u[0] = ((u64_a1 *)inp)[0] ^ tweak.u[0]; in ossl_crypto_xts128gb_encrypt()
53 scratch.u[1] = ((u64_a1 *)inp)[1] ^ tweak.u[1]; in ossl_crypto_xts128gb_encrypt()
57 scratch.u[0] ^= tweak.u[0]; in ossl_crypto_xts128gb_encrypt()
58 scratch.u[1] ^= tweak.u[1]; in ossl_crypto_xts128gb_encrypt()
61 ((u64_a1 *)out)[0] = scratch.u[0] ^= tweak.u[0]; in ossl_crypto_xts128gb_encrypt()
[all …]
/freebsd/crypto/openssl/crypto/sm4/asm/
H A Dvpsm4_ex-armv8.pl1223 my @tweak=map("v$_",(16..23));
1249 ld1 {@tweak[0].4s}, [$ivp]
1253 &rev32(@tweak[0],@tweak[0]);
1254 &encrypt_1blk(@tweak[0]);
1275 &rbit(@tweak[0],@tweak[0],$std);
1276 &rev32_armeb(@tweak[0],@tweak[0]);
1277 &mov_vec_to_reg(@tweak[0],@twx[0],@twx[1]);
1289 &mov_reg_to_vec(@twx[0],@twx[1],@tweak[0]);
1291 &mov_reg_to_vec(@twx[2],@twx[3],@tweak[1]);
1293 &mov_reg_to_vec(@twx[4],@twx[5],@tweak[2]);
[all …]
H A Dvpsm4-armv8.pl1224 my @tweak=@datax;
1249 ld1 {@tweak[0].4s}, [$ivp]
1253 &rev32(@tweak[0],@tweak[0]);
1254 &encrypt_1blk(@tweak[0]);
1275 &rbit(@tweak[0],@tweak[0],$std);
1276 &rev32_armeb(@tweak[0],@tweak[0]);
1277 &mov_vec_to_reg(@tweak[0],@twx[0],@twx[1]);
1346 &mov_reg_to_vec(@twx[8],@twx[9],@tweak[0]);
1348 &mov_reg_to_vec(@twx[10],@twx[11],@tweak[1]);
1350 &mov_reg_to_vec(@twx[12],@twx[13],@tweak[2]);
[all …]
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daesp8-ppc.pl1931 my ($tweak,$seven,$eighty7,$tmp,$tweak1) = map("v$_",(8..12));
1956 lvx $tweak,0,$ivp # load [unaligned] iv
1960 vperm $tweak,$tweak,$inptail,$inpperm
1981 vxor $tweak,$tweak,$rndkey0
1988 vcipher $tweak,$tweak,$rndkey1
1992 vcipher $tweak,$tweak,$rndkey0
1998 vcipher $tweak,$tweak,$rndkey1
2001 vcipherlast $tweak,$tweak,$rndkey0
2041 vxor $inout,$inout,$tweak
2065 vxor $rndkey0,$rndkey0,$tweak
[all …]
H A Daesni-x86_64.pl1774 my @tweak=map("%xmm$_",(10..15));
1775 my ($twmask,$twres,$twtmp)=("%xmm8","%xmm9",@tweak[4]);
1825 movdqa $inout0,@tweak[5]
1836 movdqa @tweak[5],@tweak[$i]
1838 paddq @tweak[5],@tweak[5]
1840 pxor $rndkey0,@tweak[$i]
1841 pxor $twtmp,@tweak[5]
1845 movdqa @tweak[5],@tweak[4]
1847 paddq @tweak[5],@tweak[5]
1849 pxor $rndkey0,@tweak[4]
[all …]
H A Daes-s390x.pl1642 my $tweak=16*$SIZE_T+16; # or $stdframe-16, bottom of the frame...
1661 lmg $i2,$i3,$tweak($sp) # put aside the tweak value
1667 la %r1,$tweak-16($sp)
1675 stmg $i2,$i3,$tweak($sp) # "re-seat" the tweak value
1680 lrvg $s0,$tweak+0($sp) # load the last tweak
1681 lrvg $s1,$tweak+8($sp)
1682 stmg %r0,%r3,$tweak-32($sp) # wipe copy of the key
1722 lrvg $s0,$tweak+0($s2) # load the tweak value in little-endian
1723 lrvg $s1,$tweak+8($s2)
1839 la $s2,$tweak($sp)
[all …]
H A Daesni-x86.pl1123 { my ($tweak,$twtmp,$twres,$twmask)=($rndkey1,$rndkey0,$inout0,$inout1);
1153 &movdqa ($tweak,$inout0);
1156 &pcmpgtd($twtmp,$tweak); # broadcast upper bits
1174 &movdqa (&QWP(16*$i,"esp"),$tweak);
1175 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1177 &pcmpgtd ($twtmp,$tweak); # broadcast upper bits
1178 &pxor ($tweak,$twres);
1181 &movdqa (&QWP(16*$i++,"esp"),$tweak);
1182 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1186 &pxor ($inout5,$tweak);
[all …]
H A Dbsaes-armv8.pl1482 // x4 -> key2 (used to encrypt the initial vector to yield the initial tweak)
1494 // 4*16 bytes: tweak storage across _bsaes_encrypt8
1512 // generate initial tweak
1604 str q8, [x2] // next round tweak
1618 ldr q11, [x0] // next round tweak
1706 str q18, [x0] // next round tweak
1722 ldr q11, [x0] // next round tweak
1749 ldr q11, [x0] // next round tweak
1772 ldr q11, [x0] // next round tweak
1797 mov v11.16b, v15.16b // next round tweak
[all …]
H A Dbsaes-x86_64.pl2268 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2317 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2335 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2674 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2723 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2741 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2923 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
/freebsd/sys/opencrypto/
H A Dxform_aes_xts.c97 ctx->tweak[i] = blocknum & 0xff; in aes_xts_reinit()
101 bzero(ctx->tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in aes_xts_reinit()
103 rijndael_encrypt(&ctx->key2, ctx->tweak, ctx->tweak); in aes_xts_reinit()
116 block[i] = in[i] ^ ctx->tweak[i]; in aes_xts_crypt()
124 out[i] ^= ctx->tweak[i]; in aes_xts_crypt()
129 carry_out = ctx->tweak[i] & 0x80; in aes_xts_crypt()
130 ctx->tweak[i] = (ctx->tweak[i] << 1) | (carry_in ? 1 : 0); in aes_xts_crypt()
134 ctx->tweak[0] ^= AES_XTS_ALPHA; in aes_xts_crypt()
H A Dxform_enc.h116 uint8_t tweak[AES_XTS_BLOCKSIZE]; member
/freebsd/lib/libsecureboot/
H A Dverify_file.c304 char *tweak, int *accept_no_fp) in verify_tweak() argument
306 if (strcmp(tweak, "off") == 0) { in verify_tweak()
308 } else if (strcmp(tweak, "strict") == 0) { in verify_tweak()
316 } else if (strcmp(tweak, "modules") == 0) { in verify_tweak()
319 } else if (strcmp(tweak, "try") == 0) { in verify_tweak()
322 } else if (strcmp(tweak, "verbose") == 0) { in verify_tweak()
324 } else if (strcmp(tweak, "quiet") == 0) { in verify_tweak()
327 } else if (strcmp(tweak, "silent") == 0) { in verify_tweak()
330 } else if (strncmp(tweak, "trust", 5) == 0) { in verify_tweak()
340 if (strstr(tweak, "revoke")) { in verify_tweak()
/freebsd/sys/crypto/aesni/
H A Daesni_wrap.c313 aesni_crypt_xts_block(int rounds, const __m128i *key_schedule, __m128i *tweak, in aesni_crypt_xts_block() argument
318 block = _mm_loadu_si128((const __m128i *)from) ^ *tweak; in aesni_crypt_xts_block()
325 _mm_storeu_si128((__m128i *)to, block ^ *tweak); in aesni_crypt_xts_block()
327 *tweak = xts_crank_lfsr(*tweak); in aesni_crypt_xts_block()
331 aesni_crypt_xts_block8(int rounds, const __m128i *key_schedule, __m128i *tweak, in aesni_crypt_xts_block8() argument
341 tmptweak = *tweak; in aesni_crypt_xts_block8()
363 *tweak = tmptweak; in aesni_crypt_xts_block8()
389 uint8_t tweak[AES_XTS_BLOCKSIZE] __aligned(16); in aesni_crypt_xts() local
397 bcopy(iv, tweak, AES_XTS_IVSIZE); in aesni_crypt_xts()
399 bzero(tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in aesni_crypt_xts()
[all …]
/freebsd/sys/crypto/armv8/
H A Darmv8_crypto_wrap.c218 uint8x16_t *tweak, const uint8_t *from, uint8_t *to, int do_encrypt) in armv8_aes_crypt_xts_block() argument
222 block = vld1q_u8(from) ^ *tweak; in armv8_aes_crypt_xts_block()
229 vst1q_u8(to, block ^ *tweak); in armv8_aes_crypt_xts_block()
231 *tweak = vreinterpretq_u8_s32(xts_crank_lfsr(vreinterpretq_s32_u8(*tweak))); in armv8_aes_crypt_xts_block()
242 uint8_t tweak[AES_XTS_BLOCKSIZE] __aligned(16); in armv8_aes_crypt_xts() local
254 bcopy(iv, tweak, AES_XTS_IVSIZE); in armv8_aes_crypt_xts()
256 bzero(tweak + AES_XTS_IVSIZE, AES_XTS_IVSIZE); in armv8_aes_crypt_xts()
260 tweakreg = vld1q_u8(tweak); in armv8_aes_crypt_xts()
/freebsd/crypto/openssl/providers/implementations/ciphers/
H A Dcipher_aes_xts_s390x.inc44 || ivlen > sizeof(km->tweak)) {
48 memcpy(km->tweak, iv, ivlen);
163 memcpy(xctx->base.iv, km->tweak, AES_BLOCK_SIZE);
H A Dcipher_aes_xts.h28 unsigned char tweak[16]; member
/freebsd/sys/crypto/skein/amd64/
H A Dskein_block_asm.S94 TWEAK = 8 + BCNT #tweak values[0..1]
277 StackVar ksTwk ,8*3 #key schedule: tweak words
296 StackVar bitAdd ,8 #bit count to add to tweak
/freebsd/sys/contrib/device-tree/Bindings/memory-controllers/
H A Dti-da8xx-ddrctl.txt4 a set of registers which allow to tweak the controller's behavior.
/freebsd/sys/contrib/device-tree/Bindings/sound/
H A Dcs42l42.txt77 hardware setups, a designer might want to tweak this. This is an array of
91 want to tweak default behavior.
/freebsd/crypto/openssh/
H A D.skipped-commit-ids64 b92c93266d8234d493857bb822260dacf4366157 moduli-gen.sh tweak
/freebsd/crypto/openssl/
H A DNOTES-DJGPP.md7 have to tweak the installation yourself, including renaming files
/freebsd/sys/contrib/device-tree/Bindings/soc/qcom/
H A Dqcom,glink.txt57 to tweak the default intents available for the channel to
/freebsd/sys/contrib/device-tree/src/arm/allwinner/
H A Dsun8i-h3-nanopi-duo2.dts3 * Copyright (C) 2019 Karl Palsson <karlp@tweak.net.au>
/freebsd/contrib/gdtoa/
H A Dchanges30 dtoa.c: tweak strtod (one-line addition) so the end-pointer = start
54 dtoa.c: tweak to work with 32-bit ints and 64-bit longs
182 dtoa.c: tweak to remove LL suffixes from numeric constants (for
204 dtoa.c: computationally invisible tweak for the benefit of people
233 One more tweak to omit a warning on some systems:
248 dtoa.c: tweak to bypass a bug with HUGE_VAL on HP systems.
536 dtoa.c: tweak to banish some compiler warnings.

123