Home
last modified time | relevance | path

Searched refs:tweak (Results 1 – 25 of 74) 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()
57 scratch.u[0] ^= tweak.u[0]; in CRYPTO_xts128_encrypt()
58 scratch.u[1] ^= tweak.u[1]; in CRYPTO_xts128_encrypt()
76 tweak.u[0] = (tweak.u[0] << 1) ^ res; in CRYPTO_xts128_encrypt()
77 tweak.u[1] = (tweak.u[1] << 1) | carry; in CRYPTO_xts128_encrypt()
86 tweak.c[i] = (u8)c; in CRYPTO_xts128_encrypt()
[all …]
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daesni-x86_64.pl1952 pxor @tweak[5],@tweak[0]
1968 pxor @tweak[5],@tweak[1]
1985 pxor @tweak[5],@tweak[2]
2000 pxor @tweak[5],@tweak[3]
2013 pxor @tweak[5],@tweak[4]
2439 pxor @tweak[5],@tweak[0]
2455 pxor @tweak[5],@tweak[1]
2472 pxor @tweak[5],@tweak[2]
2487 pxor @tweak[5],@tweak[3]
2500 pxor @tweak[5],@tweak[4]
[all …]
H A Daesp8-ppc.pl2090 vaddubm $tweak,$tweak,$tweak
2131 vaddubm $tweak,$tweak,$tweak
2298 vaddubm $tweak,$tweak,$tweak
2387 vaddubm $tweak,$tweak,$tweak
2530 vaddubm $tweak,$tweak,$tweak
2539 vaddubm $tweak,$tweak,$tweak
2550 vaddubm $tweak,$tweak,$tweak
2561 vaddubm $tweak,$tweak,$tweak
2572 vaddubm $tweak,$tweak,$tweak
2583 vaddubm $tweak,$tweak,$tweak
[all …]
H A Daes-s390x.pl1836 la $s2,$tweak($sp)
1932 x $s1,$tweak+4($sp)
1933 x $s2,$tweak+8($sp)
1934 x $s3,$tweak+12($sp)
2039 la $s2,$tweak($sp)
2174 x $s1,$tweak+4($sp)
2175 x $s2,$tweak+8($sp)
2176 x $s3,$tweak+12($sp)
2261 x $s1,$tweak+4($sp)
2262 x $s2,$tweak+8($sp)
[all …]
H A Daesni-x86.pl1182 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1240 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1262 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1271 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1281 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1428 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1537 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1595 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1617 &paddq ($tweak,$tweak); # &psllq($tweak,1);
1626 &paddq ($tweak,$tweak); # &psllq($tweak,1);
[all …]
H A Dbsaes-x86_64.pl2267 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2316 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2334 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2672 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2721 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2739 paddq @XMM[7], @XMM[7] # psllq 1,$tweak
2921 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/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.
H A Dcirrus,cs42l42.yaml146 For different hardware setups, a designer might want to tweak this.
184 to tweak default behavior.
/freebsd/crypto/openssh/
H A D.skipped-commit-ids54 b92c93266d8234d493857bb822260dacf4366157 moduli-gen.sh tweak
/freebsd/crypto/openssl/util/
H A Dcheck-format.pl377 my $tweak = $in_comment == -2 ? 1 : 0;
378 … report("indent = ".($count + $tweak)." != $comment_indent at end of multi-line comment")
379 if $count + $tweak != $comment_indent;
/freebsd/sys/contrib/device-tree/Bindings/remoteproc/
H A Dqcom,glink-rpm-edge.yaml63 preallocated for this virtual channel. This can be used to tweak the
/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
H A Dqcom,apr.yaml75 preallocated for this virtual channel. This can be used to tweak the
/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.
/freebsd/tools/tools/sysbuild/
H A DREADME135 # Shell functions to tweak things
/freebsd/sys/contrib/device-tree/src/arm/marvell/
H A Darmada-xp-lenovo-ix4-300d.dts228 * them up does the tweak) for poweroff to shutdown otherwise it

123