Home
last modified time | relevance | path

Searched full:tweak (Results 1 – 25 of 179) sorted by relevance

12345678

/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 …]
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daesp8-ppc.pl1922 # If $key2 is NULL, then a "tweak chaining" mode is engaged, in which #
1923 # input tweak value is assumed to be encrypted already, and last tweak #
1925 # written back to original buffer. In addition, in "tweak chaining" #
1931 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
[all …]
H A Daesni-x86_64.pl1774 my @tweak=map("%xmm$_",(10..15));
1775 my ($twmask,$twres,$twtmp)=("%xmm8","%xmm9",@tweak[4]);
1808 movups ($ivp),$inout0 # load clear-text tweak
1812 # generate the tweak
1825 movdqa $inout0,@tweak[5]
1829 # alternative tweak calculation algorithm is based on suggestions
1836 movdqa @tweak[5],@tweak[$i]
1838 paddq @tweak[5],@tweak[5]
1840 pxor $rndkey0,@tweak[$i]
1841 pxor $twtmp,@tweak[5]
[all …]
H A Daes-s390x.pl1639 my $tweak=16*$SIZE_T+16; # or $stdframe-16, bottom of the frame...
1658 lmg $i2,$i3,$tweak($sp) # put aside the tweak value
1664 la %r1,$tweak-16($sp)
1669 # with the tweak in 128-bit case.
1672 stmg $i2,$i3,$tweak($sp) # "re-seat" the tweak value
1677 lrvg $s0,$tweak+0($sp) # load the last tweak
1678 lrvg $s1,$tweak+8($sp)
1679 stmg %r0,%r3,$tweak-32($sp) # wipe copy of the key
1719 lrvg $s0,$tweak+0($s2) # load the tweak value in little-endian
1720 lrvg $s1,$tweak+8($s2)
[all …]
H A Daesni-x86.pl1123 { my ($tweak,$twtmp,$twres,$twmask)=($rndkey1,$rndkey0,$inout0,$inout1);
1127 &mov ($inp,&wparam(5)); # clear-text tweak
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);
[all …]
H A Dbsaes-x86_64.pl2229 call asm_AES_encrypt # generate initial tweak
2247 sub \$0x80, %rsp # place for tweak[8]
2248 movdqa 0x20(%rbp), @XMM[7] # initial tweak
2266 movdqa @XMM[7], `0x10*$i`(%rsp)# save tweak[$i]
2267 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2276 pxor @XMM[8+$i-2], @XMM[$i-2]# input[] ^ tweak[]
2292 pxor 0x00(%rsp), @XMM[0] # ^= tweak[]
2310 movdqa 0x70(%rsp), @XMM[7] # prepare next iteration tweak
2316 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2333 movdqa @XMM[7], `0x10*$i`(%rsp)# save tweak[$i]
[all …]
H A Dbsaes-armv7.pl1657 ldr r0, [ip] @ pointer to input tweak
1659 @ generate initial tweak
1664 mov r0,sp @ pointer to initial tweak
1673 sub r12, #`32+16` @ place for tweak[9]
1697 0: sub sp, #0x90 @ place for tweak[9]
1700 vld1.8 {@XMM[8]}, [r0] @ initial tweak
1737 vst1.64 {@XMM[8]}, [r0,:128] @ next round tweak
1770 vld1.64 {@XMM[8]}, [r0,:128] @ next round tweak
1806 vst1.64 {@XMM[15]}, [r0,:128] @ next round tweak
1837 vld1.64 {@XMM[8]}, [r0,:128] @ next round tweak
[all …]
/freebsd/sys/opencrypto/
H A Dxform_aes_xts.c92 * Prepare tweak as E_k2(IV). IV is specified as LE representation in aes_xts_reinit()
97 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()
126 /* Exponentiate tweak */ 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()
/freebsd/sys/crypto/skein/amd64/
H A Dskein_block_asm.S94 TWEAK = 8 + BCNT #tweak values[0..1] define
95 X_VARS = 16 + TWEAK #chaining vars
277 StackVar ksTwk ,8*3 #key schedule: tweak words
296 StackVar bitAdd ,8 #bit count to add to tweak
378 leaq ksTwk +F_O(%rbp),%rax #tweak pointer
466 movq TWEAK+8(%rdi),%r14
480 movq TWEAK+0(%rdi) ,%r13
481 addq bitAdd+F_O(%rbp) ,%r13 #computed updated tweak value T0
483 xorq %r13 ,%r15 #now %r13.%r15 is set as the tweak
490 movq %r13,TWEAK+0(%rdi) #save updated tweak value ctx->h.T[0]
[all …]
/freebsd/sys/contrib/device-tree/Bindings/net/
H A Dqcom,qca807x.yaml81 and qcom,dac-disable-bias-current-tweak disabled,
93 qcom,dac-disable-bias-current-tweak disabled.
96 qcom,dac-disable-bias-current-tweak:
98 Set Analog MDI driver bias current to disable tweak
101 With this not defined, bias current tweak are enabled
104 With this enabled the following tweak are NOT applied:
/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
393 * Prepare tweak as E_k2(IV). IV is specified as LE representation in aesni_crypt_xts()
397 bcopy(iv, tweak, 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
250 * Prepare tweak as E_k2(IV). IV is specified as LE representation in armv8_aes_crypt_xts()
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/sys/crypto/openssl/arm/
H A Dbsaes-armv7.S1590 ldr r0, [ip] @ pointer to input tweak
1592 @ generate initial tweak
1597 mov r0,sp @ pointer to initial tweak
1606 sub r12, #48 @ place for tweak[9]
1630 0: sub sp, #0x90 @ place for tweak[9]
1633 vld1.8 {q8}, [r0] @ initial tweak
1703 vst1.64 {q8}, [r0,:128] @ next round tweak
1736 vld1.64 {q8}, [r0,:128] @ next round tweak
1815 vst1.64 {q15}, [r0,:128] @ next round tweak
1846 vld1.64 {q8}, [r0,:128] @ next round tweak
[all …]
/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/contrib/openzfs/module/icp/algs/skein/
H A Dskein_impl.h40 /* tweak word T[1]: bit field starting positions */
55 /* tweak word T[1]: flag bit definition(s) */
60 /* tweak word T[1]: tree level bit field mask */
64 /* tweak word T[1]: block type field */
134 * Skein macros for getting/setting tweak words, etc.
148 /* set both tweak words at once */
/freebsd/sys/crypto/skein/
H A Dskein.h47 #define SKEIN_MODIFIER_WORDS ( 2) /* number of modifier (tweak) words */
70 u64b_t T[SKEIN_MODIFIER_WORDS]; /* tweak words: T[0]=byte cnt, T[1]=flags */
151 /* tweak word T[1]: bit field starting positions */
160 /* tweak word T[1]: flag bit definition(s) */
165 /* tweak word T[1]: tree level bit field mask */
169 /* tweak word T[1]: block type field */
223 ** Skein macros for getting/setting tweak words, etc.
234 /* set both tweak words at once */
/freebsd/contrib/spleen/
H A DChangeLog67 - Tweak wsfont export program to account for the new block in the 6x12 version
174 - Tweak the digit '7' for consistency with other sizes (5x8 version)
177 - Tweak the digit '2' for consistency with other sizes (12x24 version)
274 - Tweak 'f' and 't' characters to make them more consistent (8x16 version)
/freebsd/crypto/openssl/crypto/perlasm/
H A Dsparcv9_modes.pl943 ldxa [%l7]0x88, %g3 ! %g3:%g2 is tweak
1008 fxor %f12, %f0, %f0 ! ^= tweak[0]
1016 fxor %f12, %f0, %f0 ! ^= tweak[0]
1019 srax %g3, 63, %l7 ! next tweak value
1089 srax %g3, 63, %l7 ! next tweak value
1109 fxor %f12, %f0, %f0 ! ^= tweak[0]
1111 fxor %f8, %f4, %f4 ! ^= tweak[0]
1122 srax %g3, 63, %l7 ! next tweak value
1131 fxor %f12, %f0, %f0 ! ^= tweak[0]
1221 srax %g3, 63, %l7 ! next tweak value
[all …]
/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.
H A Dcirrus,cs42l42.yaml146 For different hardware setups, a designer might want to tweak this.
184 to tweak default behavior.
/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.
413 for Infinity - Infinity). Tweak test/makefile so differences in the
536 dtoa.c: tweak to banish some compiler warnings.
/freebsd/sys/contrib/openzfs/include/sys/
H A Dskein.h43 #define SKEIN_MODIFIER_WORDS (2) /* number of modifier (tweak) words */
65 /* tweak words: T[0]=byte cnt, T[1]=flags */
/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/contrib/bmake/mk/
H A Ddirdeps-targets.mk33 # This makes it feasible to tweak options like MK_DIRDEPS_CACHE
145 # some targets want to tweak options we might want to process now
/freebsd/share/mk/
H A Ddirdeps-targets.mk33 # This makes it feasible to tweak options like MK_DIRDEPS_CACHE
145 # some targets want to tweak options we might want to process now

12345678