Home
last modified time | relevance | path

Searched +full:- +full:12 +full:v (Results 1 – 25 of 1106) sorted by relevance

12345678910>>...45

/freebsd/sys/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-ref.c15 static const uint8_t blake2b_sigma[12][16] = {
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 },
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_neon.c8 #error "This implementation only supports little-endian ARM."
9 // It might be that all we need for big-endian support here is to get the loads
41 return vorrq_u32(vshrq_n_u32(x, 16), vshlq_n_u32(x, 32 - 16)); in rot16_128()
45 return vorrq_u32(vshrq_n_u32(x, 12), vshlq_n_u32(x, 32 - 12)); in rot12_128()
49 return vorrq_u32(vshrq_n_u32(x, 8), vshlq_n_u32(x, 32 - 8)); in rot8_128()
53 return vorrq_u32(vshrq_n_u32(x, 7), vshlq_n_u32(x, 32 - 7)); in rot7_128()
61 * ----------------------------------------------------------------------------
63 * ----------------------------------------------------------------------------
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()
[all …]
H A Dblake3_avx512.c57 INLINE __m128i rot12_128(__m128i x) { return _mm_ror_epi32(x, 12); } in rot12_128()
59 INLINE __m256i rot12_256(__m256i x) { return _mm256_ror_epi32(x, 12); } in rot12_256()
61 INLINE __m512i rot12_512(__m512i x) { return _mm512_ror_epi32(x, 12); } in rot12_512()
76 * ----------------------------------------------------------------------------
78 * ----------------------------------------------------------------------------
103 // discussion at https://github.com/sneves/blake2-avx2/pull/4
139 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
140 t2 = _mm_shuffle_epi32(t2, _MM_SHUFFLE(2, 1, 0, 3)); // 12 10 8 14 in compress_pre()
310 * ----------------------------------------------------------------------------
312 * ----------------------------------------------------------------------------
[all …]
H A Dblake3_avx2.c17 // Note that clang-format doesn't like the name "xor" for some reason.
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()
29 return _mm256_or_si256(_mm256_srli_epi32(x, 12), _mm256_slli_epi32(x, 32 - 12)); in rot12()
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()
39 return _mm256_or_si256(_mm256_srli_epi32(x, 7), _mm256_slli_epi32(x, 32 - 7)); in rot7()
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()
[all …]
H A Dblake3_sse41.c21 // Note that clang-format doesn't like the name "xor" for some reason.
32 x, _mm_set_epi8(13, 12, 15, 14, 9, 8, 11, 10, 5, 4, 7, 6, 1, 0, 3, 2)); in rot16()
36 return xorv(_mm_srli_epi32(x, 12), _mm_slli_epi32(x, 32 - 12)); in rot12()
41 x, _mm_set_epi8(12, 15, 14, 13, 8, 11, 10, 9, 4, 7, 6, 5, 0, 3, 2, 1)); in rot8()
45 return xorv(_mm_srli_epi32(x, 7), _mm_slli_epi32(x, 32 - 7)); in rot7()
70 // discussion at https://github.com/sneves/blake2-avx2/pull/4
106 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
107 t2 = _mm_shuffle_epi32(t2, _MM_SHUFFLE(2, 1, 0, 3)); // 12 10 8 14 in compress_pre()
276 INLINE void round_fn(__m128i v[16], __m128i m[16], size_t r) { in round_fn()
277 v[0] = addv(v[0], m[(size_t)MSG_SCHEDULE[r][0]]); in round_fn()
[all …]
H A Dblake3_sse2.c21 // Note that clang-format doesn't like the name "xor" for some reason.
35 return xorv(_mm_srli_epi32(x, 12), _mm_slli_epi32(x, 32 - 12)); in rot12()
39 return xorv(_mm_srli_epi32(x, 8), _mm_slli_epi32(x, 32 - 8)); in rot8()
43 return xorv(_mm_srli_epi32(x, 7), _mm_slli_epi32(x, 32 - 7)); in rot7()
68 // discussion at https://github.com/sneves/blake2-avx2/pull/4
112 t2 = _mm_shuffle_ps2(m2, m3, _MM_SHUFFLE(2, 0, 2, 0)); // 14 12 10 8 in compress_pre()
113 t2 = _mm_shuffle_epi32(t2, _MM_SHUFFLE(2, 1, 0, 3)); // 12 10 8 14 in compress_pre()
282 INLINE void round_fn(__m128i v[16], __m128i m[16], size_t r) { in round_fn()
283 v[0] = addv(v[0], m[(size_t)MSG_SCHEDULE[r][0]]); in round_fn()
284 v[1] = addv(v[1], m[(size_t)MSG_SCHEDULE[r][2]]); in round_fn()
[all …]
/freebsd/sys/dev/wg/
H A Dwg_crypto.c1 /* SPDX-License-Identifier: MIT
3 * Copyright (C) 2015-2021 Jason A. Donenfeld <Jason@zx2c4.com>. All Rights Reserved.
22 #define DIV_ROUND_UP(n,d) (((n) + (d) - 1) / (d))
30 while (words--) { in cpu_to_le32_array()
37 while (words--) { in le32_to_cpu_array()
44 return (word >> (shift & 31)) | (word << ((-shift) & 31)); in ror32()
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 },
[all …]
/freebsd/crypto/openssl/providers/implementations/digests/
H A Dblake2b_prov.c2 * Copyright 2016-2024 The OpenSSL Project Authors. All Rights Reserved.
32 static const uint8_t blake2b_sigma[12][16] =
34 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 } ,
35 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 } ,
36 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 } ,
37 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 } ,
38 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 } ,
39 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 } ,
40 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 } ,
41 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 } ,
[all …]
H A Dblake2s_prov.c2 * Copyright 2016-2024 The OpenSSL Project Authors. All Rights Reserved.
29 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 } ,
30 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 } ,
31 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 } ,
32 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 } ,
33 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 } ,
34 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 } ,
35 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 } ,
36 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 } ,
37 { 6, 15, 14, 9, 11, 3, 0, 8, 12, 2, 13, 7, 1, 4, 10, 5 } ,
[all …]
/freebsd/sys/contrib/libb2/
H A Dblake2b-ref.c2 BLAKE2 reference source code package - reference C implementations
19 #include "blake2-impl.h"
29 static const uint8_t blake2b_sigma[12][16] =
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 } ,
[all …]
H A Dblake2s-ref.c2 BLAKE2 reference source code package - reference C implementations
19 #include "blake2-impl.h"
29 { 0, 1, 2, 3, 4, 5, 6, 7, 8, 9, 10, 11, 12, 13, 14, 15 } ,
30 { 14, 10, 4, 8, 9, 15, 13, 6, 1, 12, 0, 2, 11, 7, 5, 3 } ,
31 { 11, 8, 12, 0, 5, 2, 15, 13, 10, 14, 3, 6, 7, 1, 9, 4 } ,
32 { 7, 9, 3, 1, 13, 12, 11, 14, 2, 6, 5, 10, 4, 0, 15, 8 } ,
33 { 9, 0, 5, 7, 2, 4, 10, 15, 14, 1, 11, 12, 6, 8, 3, 13 } ,
34 { 2, 12, 6, 10, 0, 11, 8, 3, 4, 13, 7, 5, 15, 14, 1, 9 } ,
35 { 12, 5, 1, 15, 14, 13, 4, 10, 0, 7, 6, 3, 9, 2, 8, 11 } ,
36 { 13, 11, 7, 14, 12, 1, 3, 9, 5, 0, 15, 4, 8, 6, 2, 10 } ,
[all …]
/freebsd/sys/crypto/chacha20/
H A Dchacha.c2 chacha-merged.c version 20080118
7 /* $OpenBSD: chacha.c,v 1.1 2013/11/21 00:45:44 djm Exp $ */
19 #define U8C(v) (v##U) argument
20 #define U32C(v) (v##U) argument
22 #define U8V(v) ((u8)(v) & U8C(0xFF)) argument
23 #define U32V(v) ((u32)(v) & U32C(0xFFFFFFFF)) argument
25 #define ROTL32(v, n) \ argument
26 (U32V((v) << (n)) | ((v) >> (32 - (n))))
34 #define U32TO8_LITTLE(p, v) \ argument
36 (p)[0] = U8V((v) ); \
[all …]
/freebsd/contrib/libarchive/libarchive/
H A Darchive_blake2s_ref.c2 BLAKE2 reference source code package - reference C implementations
8 - CC0 1.0 Universal : http://creativecommons.org/publicdomain/zero/1.0
9 - OpenSSL license : https://www.openssl.org/source/license.html
10 - Apache 2.0 : http://www.apache.org/licenses/LICENSE-2.0
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 } ,
[all …]
/freebsd/crypto/openssl/crypto/chacha/asm/
H A Dchacha-loongarch64.pl3 # Copyright 2023-2025 The OpenSSL Project Authors. All Rights Reserved.
17 my ($t0,$t1,$t2,$t3,$t4,$t5,$t6,$t7,$t8,$x)=map("\$r$_",(12..21));
20 # The saved floating-point registers in the LP64D ABI. In LoongArch
28 # Here is the 128-bit vector register layout for LSX extension.
34 # Here is the 256-bit vector register layout for LASX extension.
57 .ascii "expand 32-byte k"
84 addi.d $sp,$sp,-64
124 rotri.w @x[$b0],@x[$b0],20 # rotate left 12 bits
177 addi.d $sp,$sp,-256
198 ld.w @x[2],$t8,8 # '2-by'
[all …]
/freebsd/contrib/unbound/compat/
H A Dchacha_private.h2 chacha-merged.c version 20080118
7 /* $OpenBSD: chacha_private.h,v 1.2 2013/10/04 07:02:27 djm Exp $ */
17 #define U8C(v) (v##U) argument
18 #define U32C(v) (v##U) argument
20 #define U8V(v) ((u8)(v) & U8C(0xFF)) argument
21 #define U32V(v) ((u32)(v) & U32C(0xFFFFFFFF)) argument
23 #define ROTL32(v, n) \ argument
24 (U32V((v) << (n)) | ((v) >> (32 - (n))))
32 #define U32TO8_LITTLE(p, v) \ argument
34 (p)[0] = U8V((v) ); \
[all …]
/freebsd/crypto/openssh/openbsd-compat/
H A Dchacha_private.h4 chacha-merged.c version 20080118
9 /* $OpenBSD: chacha_private.h,v 1.3 2022/02/28 21:56:29 dtucker Exp $ */
19 #define U8C(v) (v##U) argument
20 #define U32C(v) (v##U) argument
22 #define U8V(v) ((u8)(v) & U8C(0xFF)) argument
23 #define U32V(v) ((u32)(v) & U32C(0xFFFFFFFF)) argument
25 #define ROTL32(v, n) \ argument
26 (U32V((v) << (n)) | ((v) >> (32 - (n))))
34 #define U32TO8_LITTLE(p, v) \ argument
36 (p)[0] = U8V((v) ); \
[all …]
/freebsd/crypto/openssh/
H A Dchacha.c1 /* $OpenBSD: chacha.c,v 1.2 2023/07/17 05:26:38 djm Exp $ */
3 chacha-merged.c version 20080118
17 #define U8C(v) (v##U) argument
18 #define U32C(v) (v##U) argument
20 #define U8V(v) ((u8)(v) & U8C(0xFF)) argument
21 #define U32V(v) ((u32)(v) & U32C(0xFFFFFFFF)) argument
23 #define ROTL32(v, n) \ argument
24 (U32V((v) << (n)) | ((v) >> (32 - (n))))
32 #define U32TO8_LITTLE(p, v) \ argument
34 (p)[0] = U8V((v) ); \
[all …]
/freebsd/bin/date/
H A Dvary.c1 /*-
43 { 9, "september" }, { 10, "october" }, { 11, "november" }, { 12, "december" },
44 { -1, NULL }
50 { -1, NULL }
61 while ((ret = mktime(t)) == -1 && t->tm_year > 68 && t->tm_year < 138) in domktime()
63 adjhour(t, type == '-' ? type : '+', 1, 0); in domktime()
73 for (f = 0; t[f].val != -1; f++) in trans()
78 return -1; in trans()
82 vary_append(struct vary *v, char *arg) in vary_append() argument
86 if (v) { in vary_append()
[all …]
/freebsd/contrib/bearssl/src/ec/
H A Dec_c25519_m15.c57 j -= k;
60 tmp[35 - k] |= (unsigned char)w;
61 tmp[34 - k] |= (unsigned char)(w >> 8);
62 tmp[33 - k] |= (unsigned char)(w >> 16);
63 tmp[32 - k] |= (unsigned char)(w >> 24);
74 * that right-shifting a signed negative integer copies the sign bit
75 * (arithmetic right-shift). This is "implementation-defined behaviour",
84 | ((-((uint32_t)(x) >> 31)) << (32 - (n))))
90 * Convert an integer from unsigned little-endian encoding to a sequence of
91 * 13-bit words in little-endian order. The final "partial" word is
[all …]
/freebsd/crypto/openssl/crypto/modes/
H A Dgcm128.c2 * Copyright 2010-2024 The OpenSSL Project Authors. All Rights Reserved.
27 # define PUTU32(p,v) *(u32 *)(p) = BSWAP4(v) argument
30 /* RISC-V uses C implementation as a fallback. */
36 #define PACK(s) ((size_t)(s)<<(sizeof(size_t)*8-16))
37 #define REDUCE1BIT(V) do { \ argument
39 u64 T = U64(0xe100000000000000) & (0-(V.lo&1)); \
40 V.lo = (V.hi<<63)|(V.lo>>1); \
41 V.hi = (V.hi>>1 )^T; \
44 u32 T = 0xe1000000U & (0-(u32)(V.lo&1)); \
45 V.lo = (V.hi<<63)|(V.lo>>1); \
[all …]
/freebsd/bin/date/tests/
H A Dformat_string_test.sh9 # These two date/times have been chosen carefully -- they
16 TEST1=3222243 # 1970-02-07 07:04:03
17 TEST2=1005600000 # 2001-11-12 21:11:12
27 atf_check -o "inline:${exp_output_1}\n" \
28 date -r ${TEST1} +%${format_string}
29 atf_check -o "inline:${exp_output_2}\n" \
30 date -r ${TEST2} +%${format_string}
40 atf_check -o "inline:$(stat -f '%9Fm' "$file")\n" \
41 date -r "$file" +%s.%N
70 atf_check -o "inline:${exp_output_1}\n" \
[all …]
/freebsd/share/man/man4/
H A Dpms.430 .Nd "PMC-Sierra PM8001/8081/8088/8089/8074/8076/8077 SAS/SATA HBA Controller driver"
35 .Bd -ragged -offset indent
42 .Bd -literal -offset indent
48 driver provides support for the PMC-Sierra PM8001/8081/8088/8089/8074/8076/8077
55 .Bl -bullet -compact
79 PMC Sierra SPC SAS-SATA Card
81 PMC Sierra SPC-V SAS-SATA Card
83 PMC Sierra SPC-VE SAS-SATA Card
85 PMC Sierra SPC-V 16 Port SAS-SATA Card
87 PMC Sierra SPC-VE 16 Port SAS-SATA Card
[all …]
/freebsd/contrib/ofed/infiniband-diags/man/
H A Dvendstat.85 VENDSTAT \-
7 .nr rst2man-indent-level 0
10 \\$1 \\n[an-margin]
11 level \\n[rst2man-indent-level]
12 level margin: \\n[rst2man-indent\\n[rst2man-indent-level]]
13 -
14 \\n[rst2man-indent0]
15 \\n[rst2man-indent1]
16 \\n[rst2man-indent2]
21 . nr rst2man-indent\\n[rst2man-indent-level] \\n[an-margin]
[all …]
H A Ddump_fts.85 DUMP_FTS \- dump InfiniBand forwarding tables
7 .nr rst2man-indent-level 0
10 \\$1 \\n[an-margin]
11 level \\n[rst2man-indent-level]
12 level margin: \\n[rst2man-indent\\n[rst2man-indent-level]]
13 -
14 \\n[rst2man-indent0]
15 \\n[rst2man-indent1]
16 \\n[rst2man-indent2]
21 . nr rst2man-indent\\n[rst2man-indent-level] \\n[an-margin]
[all …]
/freebsd/contrib/llvm-project/libcxx/src/
H A Diostream.cpp1 //===----------------------------------------------------------------------===//
5 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
7 //===----------------------------------------------------------------------===//
26 …__asm__("?cin@" _LIBCPP_ABI_NAMESPACE_STR "@std@@3V?$basic_istream@DU?$char_traits@D@" _LIBCPP_ABI…
27 "@std@@@12@A")
36 …__asm__("?wcin@" _LIBCPP_ABI_NAMESPACE_STR "@std@@3V?$basic_istream@_WU?$char_traits@_W@" _LIBCPP_…
37 "@std@@@12@A")
46 …__asm__("?cout@" _LIBCPP_ABI_NAMESPACE_STR "@std@@3V?$basic_ostream@DU?$char_traits@D@" _LIBCPP_AB…
47 "@std@@@12@A")
56 …__asm__("?wcout@" _LIBCPP_ABI_NAMESPACE_STR "@std@@3V?$basic_ostream@_WU?$char_traits@_W@" _LIBCPP…
[all …]

12345678910>>...45