/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/ |
H A D | blake3_sse41.c | 32 x, _mm_set_epi8(13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2)); in rot16() 41 x, _mm_set_epi8(12, 15, 14, 13, 8, 11, 10, 9, 4, 7, 6, 5, 0, 3, 2, 1)); in rot8() 72 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(2, 1, 0, 3)); in diagonalize() 73 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in diagonalize() 74 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(0, 3, 2, 1)); in diagonalize() 78 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(0, 3, 2, 1)); in undiagonalize() 79 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in undiagonalize() 80 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(2, 1, 0, 3)); in undiagonalize() 88 rows[2] = set4(IV[0], IV[1], IV[2], IV[3]); in compress_pre() 89 rows[3] = set4(counter_low(counter), counter_high(counter), in compress_pre() [all …]
|
H A D | blake3_sse2.c | 70 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(2, 1, 0, 3)); in diagonalize() 71 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in diagonalize() 72 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(0, 3, 2, 1)); in diagonalize() 76 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(0, 3, 2, 1)); in undiagonalize() 77 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in undiagonalize() 78 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(2, 1, 0, 3)); in undiagonalize() 94 rows[2] = set4(IV[0], IV[1], IV[2], IV[3]); in compress_pre() 95 rows[3] = set4(counter_low(counter), counter_high(counter), in compress_pre() 101 __m128i m3 = loadu(&block[sizeof(__m128i) * 3]); in compress_pre() 108 g1(&rows[0], &rows[1], &rows[2], &rows[3], t0); in compress_pre() [all …]
|
H A D | blake3_avx512.c | 105 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(2, 1, 0, 3)); in diagonalize() 106 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in diagonalize() 107 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(0, 3, 2, 1)); in diagonalize() 111 *row0 = _mm_shuffle_epi32(*row0, _MM_SHUFFLE(0, 3, 2, 1)); in undiagonalize() 112 *row3 = _mm_shuffle_epi32(*row3, _MM_SHUFFLE(1, 0, 3, 2)); in undiagonalize() 113 *row2 = _mm_shuffle_epi32(*row2, _MM_SHUFFLE(2, 1, 0, 3)); in undiagonalize() 121 rows[2] = set4(IV[0], IV[1], IV[2], IV[3]); in compress_pre() 122 rows[3] = set4(counter_low(counter), counter_high(counter), in compress_pre() 128 __m128i m3 = loadu_128(&block[sizeof(__m128i) * 3]); in compress_pre() 135 g1(&rows[0], &rows[1], &rows[2], &rows[3], t0); in compress_pre() [all …]
|
H A D | blake3_neon.c | 66 INLINE void round_fn4(uint32x4_t v[16], uint32x4_t m[16], size_t r) { in round_fn4() 67 v[0] = add_128(v[0], m[(size_t)MSG_SCHEDULE[r][0]]); in round_fn4() 68 v[1] = add_128(v[1], m[(size_t)MSG_SCHEDULE[r][2]]); in round_fn4() 69 v[2] = add_128(v[2], m[(size_t)MSG_SCHEDULE[r][4]]); in round_fn4() 70 v[3] = add_128(v[3], m[(size_t)MSG_SCHEDULE[r][6]]); in round_fn4() 71 v[0] = add_128(v[0], v[4]); in round_fn4() 72 v[1] = add_128(v[1], v[5]); in round_fn4() 73 v[2] = add_128(v[2], v[6]); in round_fn4() 74 v[3] = add_128(v[3], v[7]); in round_fn4() 75 v[12] = xor_128(v[12], v[0]); in round_fn4() [all …]
|
H A D | blake3_avx2.c | 24 x, _mm256_set_epi8(13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2, in rot16() 25 13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2)); in rot16() 34 x, _mm256_set_epi8(12, 15, 14, 13, 8, 11, 10, 9, 4, 7, 6, 5, 0, 3, 2, 1, in rot8() 35 12, 15, 14, 13, 8, 11, 10, 9, 4, 7, 6, 5, 0, 3, 2, 1)); in rot8() 42 INLINE void round_fn(__m256i v[16], __m256i m[16], size_t r) { in round_fn() 43 v[0] = addv(v[0], m[(size_t)MSG_SCHEDULE[r][0]]); in round_fn() 44 v[1] = addv(v[1], m[(size_t)MSG_SCHEDULE[r][2]]); in round_fn() 45 v[2] = addv(v[2], m[(size_t)MSG_SCHEDULE[r][4]]); in round_fn() 46 v[3] = addv(v[3], m[(size_t)MSG_SCHEDULE[r][6]]); in round_fn() 47 v[0] = addv(v[0], v[4]); in round_fn() [all …]
|
/freebsd/sys/contrib/openzfs/module/zcommon/ |
H A D | zfs_fletcher_superscalar4.c | 61 A = ctx->superscalar[0].v[0] + ctx->superscalar[0].v[1] + in fletcher_4_superscalar4_fini() 62 ctx->superscalar[0].v[2] + ctx->superscalar[0].v[3]; in fletcher_4_superscalar4_fini() 63 B = 0 - ctx->superscalar[0].v[1] - 2 * ctx->superscalar[0].v[2] - in fletcher_4_superscalar4_fini() 64 3 * ctx->superscalar[0].v[3] + 4 * ctx->superscalar[1].v[0] + in fletcher_4_superscalar4_fini() 65 4 * ctx->superscalar[1].v[1] + 4 * ctx->superscalar[1].v[2] + in fletcher_4_superscalar4_fini() 66 4 * ctx->superscalar[1].v[3]; in fletcher_4_superscalar4_fini() 68 C = ctx->superscalar[0].v[2] + 3 * ctx->superscalar[0].v[3] - in fletcher_4_superscalar4_fini() 69 6 * ctx->superscalar[1].v[0] - 10 * ctx->superscalar[1].v[1] - in fletcher_4_superscalar4_fini() 70 14 * ctx->superscalar[1].v[2] - 18 * ctx->superscalar[1].v[3] + in fletcher_4_superscalar4_fini() 71 16 * ctx->superscalar[2].v[0] + 16 * ctx->superscalar[2].v[1] + in fletcher_4_superscalar4_fini() [all …]
|
H A D | zfs_fletcher_intel.c | 61 A = ctx->avx[0].v[0] + ctx->avx[0].v[1] + in fletcher_4_avx2_fini() 62 ctx->avx[0].v[2] + ctx->avx[0].v[3]; in fletcher_4_avx2_fini() 63 B = 0 - ctx->avx[0].v[1] - 2 * ctx->avx[0].v[2] - 3 * ctx->avx[0].v[3] + in fletcher_4_avx2_fini() 64 4 * ctx->avx[1].v[0] + 4 * ctx->avx[1].v[1] + 4 * ctx->avx[1].v[2] + in fletcher_4_avx2_fini() 65 4 * ctx->avx[1].v[3]; in fletcher_4_avx2_fini() 67 C = ctx->avx[0].v[2] + 3 * ctx->avx[0].v[3] - 6 * ctx->avx[1].v[0] - in fletcher_4_avx2_fini() 68 10 * ctx->avx[1].v[1] - 14 * ctx->avx[1].v[2] - in fletcher_4_avx2_fini() 69 18 * ctx->avx[1].v[3] + 16 * ctx->avx[2].v[0] + in fletcher_4_avx2_fini() 70 16 * ctx->avx[2].v[1] + 16 * ctx->avx[2].v[2] + in fletcher_4_avx2_fini() 71 16 * ctx->avx[2].v[3]; in fletcher_4_avx2_fini() [all …]
|
H A D | zfs_fletcher_superscalar.c | 60 A = ctx->superscalar[0].v[0] + ctx->superscalar[0].v[1]; in fletcher_4_superscalar_fini() 61 B = 2 * ctx->superscalar[1].v[0] + 2 * ctx->superscalar[1].v[1] - in fletcher_4_superscalar_fini() 62 ctx->superscalar[0].v[1]; in fletcher_4_superscalar_fini() 63 C = 4 * ctx->superscalar[2].v[0] - ctx->superscalar[1].v[0] + in fletcher_4_superscalar_fini() 64 4 * ctx->superscalar[2].v[1] - 3 * ctx->superscalar[1].v[1]; in fletcher_4_superscalar_fini() 65 D = 8 * ctx->superscalar[3].v[0] - 4 * ctx->superscalar[2].v[0] + in fletcher_4_superscalar_fini() 66 8 * ctx->superscalar[3].v[1] - 8 * ctx->superscalar[2].v[1] + in fletcher_4_superscalar_fini() 67 ctx->superscalar[1].v[1]; in fletcher_4_superscalar_fini() 80 a = ctx->superscalar[0].v[0]; in fletcher_4_superscalar_native() 81 b = ctx->superscalar[1].v[0]; in fletcher_4_superscalar_native() [all …]
|
/freebsd/sys/contrib/openzfs/module/icp/asm-x86_64/aes/ |
H A D | aeskey.c | 16 * 3. the name of the copyright holder is not used to endorse products 56 * 3. Remove code under ifdef USE_VIA_ACE_IF_PRESENT (always undefined) 82 { k[4 * (i) + 4] = ss[0] ^= ls_box(ss[3], 3) ^ t_use(r, c)[i]; \ 85 k[4 * (i) + 7] = ss[3] ^= ss[2]; \ 96 rk[3] = ss[3] = word_in(key, 3); in aes_encrypt_key128() 100 ke4(rk, 2); ke4(rk, 3); in aes_encrypt_key128() 116 { k[6 * (i) + 6] = ss[0] ^= ls_box(ss[5], 3) ^ t_use(r, c)[i]; \ 119 k[6 * (i) + 9] = ss[3] ^= ss[2]; \ 124 k[6 * (i) + 10] = ss[4] ^= ss[3]; \ 136 rk[3] = ss[3] = word_in(key, 3); in aes_encrypt_key192() [all …]
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/ |
H A D | blake2b-compress-ref.c | 16 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 }, 17 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 }, 18 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 }, 19 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 }, 20 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 }, 21 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 }, 22 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 }, 23 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 }, 24 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 }, 25 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13, 0 }, [all …]
|
/freebsd/crypto/openssl/test/recipes/04-test_pem_reading_data/ |
H A D | cert-onecolumn.pem | 61 V 76 V 89 v 99 V 128 V 144 V 153 v 159 3 202 V 205 v [all …]
|
H A D | dsa-onecolumn.pem | 40 v 63 3 90 V 122 3 147 3 171 3 193 V 197 3 257 V 301 V [all …]
|
/freebsd/sys/crypto/siphash/ |
H A D | siphash.c | 13 * 3. The name of the author may not be used to endorse or promote 58 ctx->v[0] = 0x736f6d6570736575ull; in SipHash_InitX() 59 ctx->v[1] = 0x646f72616e646f6dull; in SipHash_InitX() 60 ctx->v[2] = 0x6c7967656e657261ull; in SipHash_InitX() 61 ctx->v[3] = 0x7465646279746573ull; in SipHash_InitX() 75 KASSERT(ctx->v[0] == 0x736f6d6570736575ull && in SipHash_SetKey() 82 ctx->v[0] ^= k[0]; in SipHash_SetKey() 83 ctx->v[1] ^= k[1]; in SipHash_SetKey() 84 ctx->v[ in SipHash_SetKey() [all...] |
/freebsd/contrib/byacc/test/ |
H A D | btyacc_calc1.y | 68 dreg[$1] = $3; 72 vreg[$1] = $3; 83 $$ = $1 + $3; 87 $$ = $1 - $3; 91 $$ = $1 * $3; 95 $$ = $1 / $3; 127 $$.hi = $1.hi + $3.hi; 128 $$.lo = $1.lo + $3.lo; 132 $$.hi = $1 + $3.hi; 133 $$.lo = $1 + $3.lo; [all …]
|
H A D | calc1.y | 66 dreg[$1] = $3; 70 vreg[$1] = $3; 85 $$ = $1 + $3; 89 $$ = $1 - $3; 93 $$ = $1 * $3; 97 $$ = $1 / $3; 129 $$.hi = $1.hi + $3.hi; 130 $$.lo = $1.lo + $3.lo; 134 $$.hi = $1 + $3.hi; 135 $$.lo = $1 + $3.lo; [all …]
|
H A D | varsyntax_calc1.y | 68 dreg[$1] = $3; 72 vreg[$1] = $3; 87 $$ = $1 + $3; 91 $$ = $1 - $3; 95 $$ = $1 * $3; 99 $$ = $1 / $3; 131 $$.hi = $1.hi + $3.hi; 132 $$.lo = $1.lo + $3.lo; 136 $$.hi = $1 + $3.hi; 137 $$.lo = $1 + $3.lo; [all …]
|
/freebsd/sys/powerpc/include/ |
H A D | atomic.h | 78 * atomic_add(p, v) 79 * { *p += v; } 82 #define __atomic_add_int(p, v, t) \ argument 85 " add %0, %3, %0\n" \ 89 : "r" (p), "r" (v), "m" (*p) \ 94 #define __atomic_add_long(p, v, t) \ argument 97 " add %0, %3, %0\n" \ 101 : "r" (p), "r" (v), "m" (*p) \ 105 #define __atomic_add_long(p, v, t) \ argument 108 " add %0, %3, %0\n" \ [all …]
|
/freebsd/share/doc/psd/15.yacc/ |
H A D | ssc | 192 { dreg[$1] = $3; } 194 { vreg[$1] = $3; } 203 { $$ = $1 + $3; } 205 { $$ = $1 \- $3; } 207 { $$ = $1 * $3; } 209 { $$ = $1 / $3; } 230 { $$.hi = $1.hi + $3.hi; 231 $$.lo = $1.lo + $3.lo; } 233 { $$.hi = $1 + $3.hi; 234 $$.lo = $1 + $3.lo; } [all …]
|
/freebsd/sys/dev/wg/ |
H A D | wg_crypto.c | 53 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 }, 54 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 }, 55 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 }, 56 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 }, 57 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 }, 58 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 }, 59 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 }, 60 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 }, 61 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 }, 62 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13, 0 }, [all …]
|
/freebsd/bin/sh/tests/expansion/ |
H A D | arith2.0 | 12 unset v 13 check "v=2" 2 14 check "v" 2 15 check "$(($v))" 2 16 check "v+=1" 3 17 check "v" 3 27 v=42 28 check "!v" 0 29 check "!!v" 1 34 check "-v" -42 [all …]
|
/freebsd/crypto/openssl/providers/implementations/digests/ |
H A D | blake2b_prov.c | 33 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 } , 34 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 } , 35 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 } , 36 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 } , 37 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 } , 38 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 } , 39 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 } , 40 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 } , 41 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 } , 42 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13 , 0 } , [all …]
|
H A D | blake2s_prov.c | 31 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 } , 32 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 } , 33 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 } , 34 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 } , 35 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 } , 36 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 } , 37 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 } , 38 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 } , 39 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 } , 40 { 10, 2, 8, 4, 7, 6, 1, 5, 15, 11, 9, 14, 3, 12, 13 , 0 } , [all …]
|
/freebsd/contrib/bc/tests/bc/ |
H A D | errors.txt | 5 3 $ 7 13 a(3,3 16 3 + 17 3 - - 28 "s" + 3 29 3 - "o" 31 "3" / "2" 32 !"3" 36 * 3 37 + 4 + 3 [all …]
|
/freebsd/sys/opencrypto/ |
H A D | gfmult.c | 40 /* calculate v * 2 */ 42 gf128_mulalpha(struct gf128 v) in gf128_mulalpha() argument 46 mask = !!(v.v[1] & 1); in gf128_mulalpha() 48 v.v[1] = (v.v[1] >> 1) | ((v.v[0] & 1) << 63); in gf128_mulalpha() 49 v.v[0] = (v.v[0] >> 1) ^ ((mask & REV_POLY_REDUCT) << 56); in gf128_mulalpha() 51 return v; in gf128_mulalpha() 73 t->a[nib_rev[i]] = tbl[i].v[0] >> 32; in gf128_genmultable() 74 t->b[nib_rev[i]] = tbl[i].v[0]; in gf128_genmultable() 75 t->c[nib_rev[i]] = tbl[i].v[1] >> 32; in gf128_genmultable() 76 t->d[nib_rev[i]] = tbl[i].v[1]; in gf128_genmultable() [all …]
|
/freebsd/sys/contrib/libsodium/src/libsodium/crypto_scalarmult/curve25519/sandy2x/ |
H A D | curve25519_sandy2x.c | 29 fe var[3]; in crypto_scalarmult_curve25519_sandy2x() 45 z_51.v[0] = (z2[1] << 26) + z2[0]; in crypto_scalarmult_curve25519_sandy2x() 46 z_51.v[1] = (z2[3] << 26) + z2[2]; in crypto_scalarmult_curve25519_sandy2x() 47 z_51.v[2] = (z2[5] << 26) + z2[4]; in crypto_scalarmult_curve25519_sandy2x() 48 z_51.v[3] = (z2[7] << 26) + z2[6]; in crypto_scalarmult_curve25519_sandy2x() 49 z_51.v[4] = (z2[9] << 26) + z2[8]; in crypto_scalarmult_curve25519_sandy2x() 51 x_51.v[0] = (x2[1] << 26) + x2[0]; in crypto_scalarmult_curve25519_sandy2x() 52 x_51.v[1] = (x2[3] << 26) + x2[2]; in crypto_scalarmult_curve25519_sandy2x() 53 x_51.v[2] = (x2[5] << 26) + x2[4]; in crypto_scalarmult_curve25519_sandy2x() 54 x_51.v[3] = (x2[7] << 26) + x2[6]; in crypto_scalarmult_curve25519_sandy2x() [all …]
|