/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 | 62 A = ctx->superscalar[0].v[0] + ctx->superscalar[0].v[1] + in fletcher_4_superscalar4_fini() 63 ctx->superscalar[0].v[2] + ctx->superscalar[0].v[3]; in fletcher_4_superscalar4_fini() 64 B = 0 - ctx->superscalar[0].v[1] - 2 * ctx->superscalar[0].v[2] - in fletcher_4_superscalar4_fini() 65 3 * ctx->superscalar[0].v[3] + 4 * ctx->superscalar[1].v[0] + in fletcher_4_superscalar4_fini() 66 4 * ctx->superscalar[1].v[1] + 4 * ctx->superscalar[1].v[2] + in fletcher_4_superscalar4_fini() 67 4 * ctx->superscalar[1].v[3]; in fletcher_4_superscalar4_fini() 69 C = ctx->superscalar[0].v[2] + 3 * ctx->superscalar[0].v[3] - in fletcher_4_superscalar4_fini() 70 6 * ctx->superscalar[1].v[0] - 10 * ctx->superscalar[1].v[1] - in fletcher_4_superscalar4_fini() 71 14 * ctx->superscalar[1].v[2] - 18 * ctx->superscalar[1].v[3] + in fletcher_4_superscalar4_fini() 72 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 | 62 A = ctx->avx[0].v[0] + ctx->avx[0].v[1] + in fletcher_4_avx2_fini() 63 ctx->avx[0].v[2] + ctx->avx[0].v[3]; in fletcher_4_avx2_fini() 64 B = 0 - ctx->avx[0].v[1] - 2 * ctx->avx[0].v[2] - 3 * ctx->avx[0].v[3] + in fletcher_4_avx2_fini() 65 4 * ctx->avx[1].v[0] + 4 * ctx->avx[1].v[1] + 4 * ctx->avx[1].v[2] + in fletcher_4_avx2_fini() 66 4 * ctx->avx[1].v[3]; in fletcher_4_avx2_fini() 68 C = ctx->avx[0].v[2] + 3 * ctx->avx[0].v[3] - 6 * ctx->avx[1].v[0] - in fletcher_4_avx2_fini() 69 10 * ctx->avx[1].v[1] - 14 * ctx->avx[1].v[2] - in fletcher_4_avx2_fini() 70 18 * ctx->avx[1].v[3] + 16 * ctx->avx[2].v[0] + in fletcher_4_avx2_fini() 71 16 * ctx->avx[2].v[1] + 16 * ctx->avx[2].v[2] + in fletcher_4_avx2_fini() 72 16 * ctx->avx[2].v[3]; in fletcher_4_avx2_fini() [all …]
|
H A D | zfs_fletcher_superscalar.c | 61 A = ctx->superscalar[0].v[0] + ctx->superscalar[0].v[1]; in fletcher_4_superscalar_fini() 62 B = 2 * ctx->superscalar[1].v[0] + 2 * ctx->superscalar[1].v[1] - in fletcher_4_superscalar_fini() 63 ctx->superscalar[0].v[1]; in fletcher_4_superscalar_fini() 64 C = 4 * ctx->superscalar[2].v[0] - ctx->superscalar[1].v[0] + in fletcher_4_superscalar_fini() 65 4 * ctx->superscalar[2].v[1] - 3 * ctx->superscalar[1].v[1]; in fletcher_4_superscalar_fini() 66 D = 8 * ctx->superscalar[3].v[0] - 4 * ctx->superscalar[2].v[0] + in fletcher_4_superscalar_fini() 67 8 * ctx->superscalar[3].v[1] - 8 * ctx->superscalar[2].v[1] + in fletcher_4_superscalar_fini() 68 ctx->superscalar[1].v[1]; in fletcher_4_superscalar_fini() 81 a = ctx->superscalar[0].v[0]; in fletcher_4_superscalar_native() 82 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 | 1 // SPDX-License-Identifier: Brian-Gladman-3-Clause 17 * 3. the name of the copyright holder is not used to endorse products 57 * 3. Remove code under ifdef USE_VIA_ACE_IF_PRESENT (always undefined) 83 { k[4 * (i) + 4] = ss[0] ^= ls_box(ss[3], 3) ^ t_use(r, c)[i]; \ 86 k[4 * (i) + 7] = ss[3] ^= ss[2]; \ 97 rk[3] = ss[3] = word_in(key, 3); in aes_encrypt_key128() 101 ke4(rk, 2); ke4(rk, 3); in aes_encrypt_key128() 117 { k[6 * (i) + 6] = ss[0] ^= ls_box(ss[5], 3) ^ t_use(r, c)[i]; \ 120 k[6 * (i) + 9] = ss[3] ^= ss[2]; \ 125 k[6 * (i) + 10] = ss[4] ^= ss[3]; \ [all …]
|
/freebsd/crypto/krb5/src/lib/crypto/builtin/aes/ |
H A D | aeskey.c | 86 { k[4*(i)+4] = ss[0] ^= ls_box(ss[3],3) ^ t_use(r,c)[i]; \ 89 k[4*(i)+7] = ss[3] ^= ss[2]; \ 98 cx->ks[3] = ss[3] = word_in(key, 3); in aes_xi() 102 ke4(cx->ks, 2); ke4(cx->ks, 3); in aes_xi() 129 { k[6*(i)+ 6] = ss[0] ^= ls_box(ss[5],3) ^ t_use(r,c)[i]; \ 132 k[6*(i)+ 9] = ss[3] ^= ss[2]; \ 137 k[6*(i)+10] = ss[4] ^= ss[3]; \ 147 cx->ks[3] = ss[3] = word_in(key, 3); in aes_xi() 153 ke6(cx->ks, 2); ke6(cx->ks, 3); in aes_xi() 179 { k[8*(i)+ 8] = ss[0] ^= ls_box(ss[7],3) ^ t_use(r,c)[i]; \ [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/crypto/krb5/doc/html/ |
H A D | objects.inv | 3 # Version: 1.21.3 8 3W�������t�>k�� 13 …�g��,s��G�,{e2��M&�z?�R;9{�b��T�G�p��fyҨ��JCX��������u�{k�+��y�mb�:3FZb:&�\B�u3 �C5��<�… 15 �%�cr��%$��0]HY��ȹ�����IM��( ��U>K�L��θ�hr�Yl�T�T���v�2��̡�w�C��3o�s��l�()i���$-s�UOS|Ʉ��G 16 …}�D^�F�ô�,�i��3Z���v�r�����L���&���ڡ��vhgY����[��;u��T�鬻��(|�(-����Q�%)^��N���#s�'���… 17 ��LA�3L�DH�(�\B��[܀z;u@���"��Q�v����T�u��:n@��>��b�����q;À�A�$V�Y��ۢ����u�3X�����LQD���dJ0Q… 20 …0�g�0)��Ť��CF���� �酪��r�"Ify��o)<(��H:z>��s���xt�P�e���ccp��h��S�p���1-jg3%�g�2%�疒^ 23 …����C�L�J���Q�NT0t²"ѰLj�������mA^\�%���3S�i&^';D+�'����}<(��H�Ɍ��b2�qS���=.�W,6�ʹ��… 28 ��H��T���F�-[�Xy�6�2�=�b0��K��z�?����HO��v�nW4?��9�!48�9��Cr����@���ऒT�W�GF*��J���o6ٮ… 29 �vBD)9�D�GM�;buIe�~������ȴ'�R7<��7�۸� 8(5�G������HĞ�G�hMf#v���Ǧ�X��a� �H��C���s*;m�wV�����L… [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/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/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/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 …]
|