Home
last modified time | relevance | path

Searched refs:S (Results 1 – 25 of 310) sorted by relevance

12345678910>>...13

/f-stack/app/redis-5.0.5/deps/lua/src/
H A Dlundump.c43 #define LoadMem(S,b,n,size) LoadBlock(S,b,(n)*(size)) argument
44 #define LoadByte(S) (lu_byte)LoadChar(S) argument
45 #define LoadVar(S,x) LoadMem(S,&x,1,sizeof(x)) argument
46 #define LoadVector(S,b,n,size) LoadMem(S,b,n,size) argument
57 LoadVar(S,x); in LoadChar()
84 char* s=luaZ_openspace(S->L,S->b,size); in LoadString()
123 setsvalue2n(S->L,o,LoadString(S)); in LoadConstants()
166 setptvalue2s(S->L,S->L->top,f); incr_top(S->L); in LoadFunction()
204 S.L=L; in luaU_undump()
205 S.Z=Z; in luaU_undump()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-ref.c65 uint128_t t = ((uint128_t) S->t[1] << 64) | S->t[0]; in blake2b_increment_counter()
71 S->t[1] += (S->t[0] < inc); in blake2b_increment_counter()
118 S->h[i] ^= LOAD64_LE(p + sizeof(S->h[i]) * i); in blake2b_init_param()
271 blake2b_compress(S, S->buf); /* Compress */ in blake2b_update()
302 blake2b_compress(S, S->buf); in blake2b_final()
305 memcpy(S->buf, S->buf + BLAKE2B_BLOCKBYTES, S->buflen); in blake2b_final()
308 blake2b_increment_counter(S, S->buflen); in blake2b_final()
310 memset(S->buf + S->buflen, 0, in blake2b_final()
312 blake2b_compress(S, S->buf); in blake2b_final()
325 sodium_memzero(S->h, sizeof S->h); in blake2b_final()
[all …]
H A Dblake2b-compress-sse41.c35 blake2b_compress_sse41(blake2b_state *S, in blake2b_compress_sse41() argument
56 row1l = LOADU(&S->h[0]); in blake2b_compress_sse41()
57 row1h = LOADU(&S->h[2]); in blake2b_compress_sse41()
58 row2l = LOADU(&S->h[4]); in blake2b_compress_sse41()
59 row2h = LOADU(&S->h[6]); in blake2b_compress_sse41()
62 row4l = _mm_xor_si128(LOADU(&blake2b_IV[4]), LOADU(&S->t[0])); in blake2b_compress_sse41()
63 row4h = _mm_xor_si128(LOADU(&blake2b_IV[6]), LOADU(&S->f[0])); in blake2b_compress_sse41()
78 STOREU(&S->h[0], _mm_xor_si128(LOADU(&S->h[0]), row1l)); in blake2b_compress_sse41()
79 STOREU(&S->h[2], _mm_xor_si128(LOADU(&S->h[2]), row1h)); in blake2b_compress_sse41()
82 STOREU(&S->h[4], _mm_xor_si128(LOADU(&S->h[4]), row2l)); in blake2b_compress_sse41()
[all …]
H A Dblake2b-compress-ssse3.c29 blake2b_compress_ssse3(blake2b_state *S, in blake2b_compress_ssse3() argument
59 row1l = LOADU(&S->h[0]); in blake2b_compress_ssse3()
60 row1h = LOADU(&S->h[2]); in blake2b_compress_ssse3()
61 row2l = LOADU(&S->h[4]); in blake2b_compress_ssse3()
62 row2h = LOADU(&S->h[6]); in blake2b_compress_ssse3()
65 row4l = _mm_xor_si128(LOADU(&blake2b_IV[4]), LOADU(&S->t[0])); in blake2b_compress_ssse3()
66 row4h = _mm_xor_si128(LOADU(&blake2b_IV[6]), LOADU(&S->f[0])); in blake2b_compress_ssse3()
81 STOREU(&S->h[0], _mm_xor_si128(LOADU(&S->h[0]), row1l)); in blake2b_compress_ssse3()
82 STOREU(&S->h[2], _mm_xor_si128(LOADU(&S->h[2]), row1h)); in blake2b_compress_ssse3()
85 STOREU(&S->h[4], _mm_xor_si128(LOADU(&S->h[4]), row2l)); in blake2b_compress_ssse3()
[all …]
H A Dblake2b-compress-avx2.c38 blake2b_compress_avx2(blake2b_state *S, const uint8_t block[BLAKE2B_BLOCKBYTES]) in blake2b_compress_avx2() argument
40 __m256i a = LOADU(&S->h[0]); in blake2b_compress_avx2()
41 __m256i b = LOADU(&S->h[4]); in blake2b_compress_avx2()
42 BLAKE2B_COMPRESS_V1(a, b, block, S->t[0], S->t[1], S->f[0], S->f[1]); in blake2b_compress_avx2()
43 STOREU(&S->h[0], a); in blake2b_compress_avx2()
44 STOREU(&S->h[4], b); in blake2b_compress_avx2()
H A Dblake2.h77 int blake2b_init(blake2b_state *S, const uint8_t outlen);
78 int blake2b_init_salt_personal(blake2b_state *S, const uint8_t outlen,
82 int blake2b_init_key_salt_personal(blake2b_state *S, const uint8_t outlen,
85 int blake2b_init_param(blake2b_state *S, const blake2b_param *P);
86 int blake2b_update(blake2b_state *S, const uint8_t *in, uint64_t inlen);
87 int blake2b_final(blake2b_state *S, uint8_t *out, uint8_t outlen);
97 typedef int (*blake2b_compress_fn)(blake2b_state *S,
100 int blake2b_compress_ref(blake2b_state *S,
102 int blake2b_compress_ssse3(blake2b_state *S,
104 int blake2b_compress_sse41(blake2b_state *S,
[all …]
/f-stack/freebsd/contrib/libb2/
H A Dblake2b.c89 S->f[1] = 0ULL; in blake2b_clear_lastnode()
95 if( S->last_node ) blake2b_set_lastnode( S ); in blake2b_set_lastblock()
103 if( S->last_node ) blake2b_clear_lastnode( S ); in blake2b_clear_lastblock()
114 __uint128_t t = ( ( __uint128_t )S->t[1] << 64 ) | S->t[0]; in blake2b_increment_counter()
120 S->t[1] += ( S->t[0] < inc ); in blake2b_increment_counter()
370 blake2b_compress( S, S->buf ); // Compress in blake2b_update()
396 blake2b_compress( S, S->buf ); in blake2b_final()
398 memcpy( S->buf, S->buf + BLAKE2B_BLOCKBYTES, S->buflen ); in blake2b_final()
401 blake2b_increment_counter( S, S->buflen ); in blake2b_final()
403 memset( S->buf + S->buflen, 0, 2 * BLAKE2B_BLOCKBYTES - S->buflen ); /* Padding */ in blake2b_final()
[all …]
H A Dblake2b-ref.c61 if( S->last_node ) blake2b_set_lastnode( S ); in blake2b_set_lastblock()
69 if( S->last_node ) blake2b_clear_lastnode( S ); in blake2b_clear_lastblock()
78 S->t[1] += ( S->t[0] < inc ); in blake2b_increment_counter()
176 S->h[i] ^= load64( p + sizeof( S->h[i] ) * i ); in blake2b_init_param()
293 S->h[i] = S->h[i] ^ v[i] ^ v[i + 8]; in blake2b_compress()
313 blake2b_compress( S, S->buf ); // Compress in blake2b_update()
341 blake2b_compress( S, S->buf ); in blake2b_final()
343 memcpy( S->buf, S->buf + BLAKE2B_BLOCKBYTES, S->buflen ); in blake2b_final()
346 blake2b_increment_counter( S, S->buflen ); in blake2b_final()
348 memset( S->buf + S->buflen, 0, 2 * BLAKE2B_BLOCKBYTES - S->buflen ); /* Padding */ in blake2b_final()
[all …]
H A Dblake2s-ref.c49 S->f[1] = 0U; in blake2s_clear_lastnode()
56 if( S->last_node ) blake2s_set_lastnode( S ); in blake2s_set_lastblock()
64 if( S->last_node ) blake2s_clear_lastnode( S ); in blake2s_clear_lastblock()
66 S->f[0] = 0U; in blake2s_clear_lastblock()
73 S->t[1] += ( S->t[0] < inc ); in blake2s_increment_counter()
283 S->h[i] = S->h[i] ^ v[i] ^ v[i + 8]; in blake2s_compress()
303 blake2s_compress( S, S->buf ); // Compress in blake2s_update()
331 blake2s_compress( S, S->buf ); in blake2s_final()
333 memcpy( S->buf, S->buf + BLAKE2S_BLOCKBYTES, S->buflen ); in blake2s_final()
338 memset( S->buf + S->buflen, 0, 2 * BLAKE2S_BLOCKBYTES - S->buflen ); /* Padding */ in blake2s_final()
[all …]
H A Dblake2s.c84 S->f[1] = 0U; in blake2s_clear_lastnode()
90 if( S->last_node ) blake2s_set_lastnode( S ); in blake2s_set_lastblock()
98 if( S->last_node ) blake2s_clear_lastnode( S ); in blake2s_clear_lastblock()
100 S->f[0] = 0U; in blake2s_clear_lastblock()
106 uint64_t t = ( ( uint64_t )S->t[1] << 32 ) | S->t[0]; in blake2s_increment_counter()
343 blake2s_compress( S, S->buf ); // Compress in blake2s_update()
371 blake2s_compress( S, S->buf ); in blake2s_final()
373 memcpy( S->buf, S->buf + BLAKE2S_BLOCKBYTES, S->buflen ); in blake2s_final()
378 memset( S->buf + S->buflen, 0, 2 * BLAKE2S_BLOCKBYTES - S->buflen ); /* Padding */ in blake2s_final()
379 blake2s_compress( S, S->buf ); in blake2s_final()
[all …]
H A Dblake2sp.c68 memset( S->buf, 0, sizeof( S->buf ) ); in blake2sp_init()
69 S->buflen = 0; in blake2sp_init()
78 S->S[PARALLELISM_DEGREE - 1]->last_node = 1; in blake2sp_init()
89 memset( S->buf, 0, sizeof( S->buf ) ); in blake2sp_init_key()
90 S->buflen = 0; in blake2sp_init_key()
100 S->S[PARALLELISM_DEGREE - 1]->last_node = 1; in blake2sp_init_key()
108 blake2s_update( S->S[i], block, BLAKE2S_BLOCKBYTES ); in blake2sp_init_key()
126 blake2s_update( S->S[i], S->buf + i * BLAKE2S_BLOCKBYTES, BLAKE2S_BLOCKBYTES ); in blake2sp_update()
149 blake2s_update( S->S[id__], in__, BLAKE2S_BLOCKBYTES ); in blake2sp_update()
180 blake2s_update( S->S[i], S->buf + i * BLAKE2S_BLOCKBYTES, left ); in blake2sp_final()
[all …]
H A Dblake2bp.c71 memset( S->buf, 0, sizeof( S->buf ) ); in blake2bp_init()
72 S->buflen = 0; in blake2bp_init()
81 S->S[PARALLELISM_DEGREE - 1]->last_node = 1; in blake2bp_init()
92 memset( S->buf, 0, sizeof( S->buf ) ); in blake2bp_init_key()
93 S->buflen = 0; in blake2bp_init_key()
103 S->S[PARALLELISM_DEGREE - 1]->last_node = 1; in blake2bp_init_key()
111 blake2b_update( S->S[i], block, BLAKE2B_BLOCKBYTES ); in blake2bp_init_key()
129 blake2b_update( S->S[i], S->buf + i * BLAKE2B_BLOCKBYTES, BLAKE2B_BLOCKBYTES ); in blake2bp_update()
152 blake2b_update( S->S[id__], in__, BLAKE2B_BLOCKBYTES ); in blake2bp_update()
184 blake2b_update( S->S[i], S->buf + i * BLAKE2B_BLOCKBYTES, left ); in blake2bp_final()
[all …]
H A Dblake2-dispatch.c449 return blake2b_init_ptr( S, outlen ); in blake2b_init_dispatch()
461 return blake2b_init_param_ptr( S, P ); in blake2b_init_param_dispatch()
467 return blake2b_update_ptr( S, in, inlen ); in blake2b_update_dispatch()
484 return blake2b_init_ptr( S, outlen ); in blake2b_init()
494 return blake2b_init_param_ptr( S, P ); in blake2b_init_param()
499 return blake2b_update_ptr( S, in, inlen ); in blake2b_update()
515 return blake2s_init_ptr( S, outlen ); in blake2s_init_dispatch()
527 return blake2s_init_param_ptr( S, P ); in blake2s_init_param_dispatch()
533 return blake2s_update_ptr( S, in, inlen ); in blake2s_update_dispatch()
550 return blake2s_init_ptr( S, outlen ); in blake2s_init()
[all …]
H A Dblake2.h125 blake2s_state S[8][1]; member
134 blake2b_state S[4][1]; member
143 BLAKE2_API int blake2s_init( blake2s_state *S, size_t outlen );
145 BLAKE2_API int blake2s_init_param( blake2s_state *S, const blake2s_param *P );
147 BLAKE2_API int blake2s_final( blake2s_state *S, uint8_t *out, size_t outlen );
149 BLAKE2_API int blake2b_init( blake2b_state *S, size_t outlen );
151 BLAKE2_API int blake2b_init_param( blake2b_state *S, const blake2b_param *P );
153 BLAKE2_API int blake2b_final( blake2b_state *S, uint8_t *out, size_t outlen );
155 BLAKE2_API int blake2sp_init( blake2sp_state *S, size_t outlen );
158 BLAKE2_API int blake2sp_final( blake2sp_state *S, uint8_t *out, size_t outlen );
[all …]
/f-stack/freebsd/contrib/ck/include/gcc/x86/
H A Dck_pr.h125 #define CK_PR_FAS_S(S, T, I) CK_PR_FAS(S, T, T, T, I) argument
151 #define CK_PR_LOAD_S(S, T, I) CK_PR_LOAD(S, T, T, T, I) argument
176 #define CK_PR_STORE_S(S, T, I) CK_PR_STORE(S, T, T, T, I) argument
205 #define CK_PR_FAA_S(S, T, I) CK_PR_FAA(S, T, T, T, I) argument
222 CK_PR_UNARY_V(K, S, T, C, I)
226 ck_pr_##K##_##S(T *target) \
248 #define CK_PR_UNARY_S(K, S, T, I) CK_PR_UNARY(K, S, T, T, I) argument
288 #define CK_PR_BINARY_S(K, S, T, I) CK_PR_BINARY(K, S, T, T, T, I) argument
328 #define CK_PR_CAS_S(S, T, I) CK_PR_CAS(S, T, T, T, I) argument
363 CK_PR_CAS_O(S, T, T, T, I, R)
[all …]
/f-stack/freebsd/contrib/ck/include/gcc/
H A Dck_pr.h58 #define CK_PR_LOAD(S, M, T) \ argument
99 #define CK_PR_LOAD_S(S, T) CK_PR_LOAD(S, T, T) argument
167 #define CK_PR_CAS_S(S, T) CK_PR_CAS(S, T, T) argument
191 #define CK_PR_CAS_O(S, T) \ argument
213 #define CK_PR_FAA(S, M, T) \ argument
223 #define CK_PR_FAA_S(S, T) CK_PR_FAA(S, T, T) argument
247 #define CK_PR_BINARY_S(K, S, T) CK_PR_BINARY(K, S, T, T) argument
269 #define CK_PR_UNARY(S, M, T) \ argument
271 ck_pr_inc_##S(M *target) \
277 ck_pr_dec_##S(M *target) \
[all …]
/f-stack/freebsd/contrib/ck/include/gcc/x86_64/
H A Dck_pr.h154 #define CK_PR_FAS_S(S, T, I) CK_PR_FAS(S, T, T, T, I) argument
187 #define CK_PR_LOAD_S(S, T, I) CK_PR_LOAD(S, T, T, T, I) argument
272 #define CK_PR_STORE_S(S, T, I, K) CK_PR_STORE_IMM(S, T, T, T, I, K) argument
303 #define CK_PR_FAA_S(S, T, I) CK_PR_FAA(S, T, T, T, I) argument
321 CK_PR_UNARY_V(K, S, T, C, I)
325 ck_pr_##K##_##S(T *target) \
347 #define CK_PR_UNARY_S(K, S, T, I) CK_PR_UNARY(K, S, T, T, I) argument
388 #define CK_PR_BINARY_S(K, S, T, I, O) CK_PR_BINARY(K, S, T, T, T, I, O) argument
429 #define CK_PR_CAS_S(S, T, I) CK_PR_CAS(S, T, T, T, I) argument
468 CK_PR_CAS_O(S, T, T, T, I, R)
[all …]
/f-stack/dpdk/drivers/net/ixgbe/base/
H A Dixgbe_osdep.h30 #define DEBUGOUT(S, args...) PMD_DRV_LOG_RAW(DEBUG, S, ##args) argument
31 #define DEBUGOUT1(S, args...) DEBUGOUT(S, ##args) argument
32 #define DEBUGOUT2(S, args...) DEBUGOUT(S, ##args) argument
33 #define DEBUGOUT3(S, args...) DEBUGOUT(S, ##args) argument
34 #define DEBUGOUT6(S, args...) DEBUGOUT(S, ##args) argument
35 #define DEBUGOUT7(S, args...) DEBUGOUT(S, ##args) argument
37 #define ERROR_REPORT1(e, S, args...) DEBUGOUT(S, ##args) argument
38 #define ERROR_REPORT2(e, S, args...) DEBUGOUT(S, ##args) argument
39 #define ERROR_REPORT3(e, S, args...) DEBUGOUT(S, ##args) argument
48 #define EWARN(hw, S, args...) DEBUGOUT1(S, ##args) argument
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_hash/sha512/cp/
H A Dhash_sha512_cp.c105 RND(S[(80 - i) % 8], S[(81 - i) % 8], S[(82 - i) % 8], S[(83 - i) % 8], \
106 S[(84 - i) % 8], S[(85 - i) % 8], S[(86 - i) % 8], S[(87 - i) % 8], \
120 memcpy(S, state, 64); in SHA512_Transform()
122 RNDr(S, W, 0, i); in SHA512_Transform()
123 RNDr(S, W, 1, i); in SHA512_Transform()
124 RNDr(S, W, 2, i); in SHA512_Transform()
125 RNDr(S, W, 3, i); in SHA512_Transform()
126 RNDr(S, W, 4, i); in SHA512_Transform()
127 RNDr(S, W, 5, i); in SHA512_Transform()
128 RNDr(S, W, 6, i); in SHA512_Transform()
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_hash/sha256/cp/
H A Dhash_sha256_cp.c89 RND(S[(64 - i) % 8], S[(65 - i) % 8], S[(66 - i) % 8], S[(67 - i) % 8], \
90 S[(68 - i) % 8], S[(69 - i) % 8], S[(70 - i) % 8], S[(71 - i) % 8], \
104 memcpy(S, state, 32); in SHA256_Transform()
106 RNDr(S, W, 0, i); in SHA256_Transform()
107 RNDr(S, W, 1, i); in SHA256_Transform()
108 RNDr(S, W, 2, i); in SHA256_Transform()
109 RNDr(S, W, 3, i); in SHA256_Transform()
110 RNDr(S, W, 4, i); in SHA256_Transform()
111 RNDr(S, W, 5, i); in SHA256_Transform()
112 RNDr(S, W, 6, i); in SHA256_Transform()
[all …]
/f-stack/freebsd/tools/fdt/
H A Dmake_dtb.sh6 S=$1
26 …S/contrib/device-tree/include" -I "$S/dts/${MACHINE}" -I "$S/contrib/device-tree/src/${MACHINE}" -…
27 …DTC} -@ -O dtb -o "$dtb" -b 0 -p 1024 -i "$S/dts/${MACHINE}" -i "$S/contrib/device-tree/src/${MACH…
/f-stack/freebsd/contrib/openzfs/module/os/freebsd/spl/
H A Dsha256c.c122 RND(S[(64 - i) % 8], S[(65 - i) % 8], \
123 S[(66 - i) % 8], S[(67 - i) % 8], \
124 S[(68 - i) % 8], S[(69 - i) % 8], \
125 S[(70 - i) % 8], S[(71 - i) % 8], \
141 uint32_t S[8]; in SHA256_Transform() local
152 RNDr(S, W, 0, i); in SHA256_Transform()
153 RNDr(S, W, 1, i); in SHA256_Transform()
154 RNDr(S, W, 2, i); in SHA256_Transform()
155 RNDr(S, W, 3, i); in SHA256_Transform()
156 RNDr(S, W, 4, i); in SHA256_Transform()
[all …]
/f-stack/freebsd/crypto/sha2/
H A Dsha256c.c120 RND(S[(64 - i) % 8], S[(65 - i) % 8], \
121 S[(66 - i) % 8], S[(67 - i) % 8], \
122 S[(68 - i) % 8], S[(69 - i) % 8], \
123 S[(70 - i) % 8], S[(71 - i) % 8], \
138 uint32_t S[8]; in SHA256_Transform() local
149 RNDr(S, W, 0, i); in SHA256_Transform()
150 RNDr(S, W, 1, i); in SHA256_Transform()
151 RNDr(S, W, 2, i); in SHA256_Transform()
152 RNDr(S, W, 3, i); in SHA256_Transform()
153 RNDr(S, W, 4, i); in SHA256_Transform()
[all …]
/f-stack/freebsd/contrib/ck/include/gcc/aarch64/
H A Dck_pr.h90 #define CK_PR_LOAD(S, M, T, I) \ argument
92 ck_pr_md_load_##S(const M *target) \
101 #define CK_PR_LOAD_64(S, M, T, I) \ argument
103 ck_pr_md_load_##S(const M *target) \
116 #define CK_PR_LOAD_S(S, T, I) CK_PR_LOAD(S, T, T, I) argument
117 #define CK_PR_LOAD_S_64(S, T, I) CK_PR_LOAD_64(S, T, T, I) argument
136 #define CK_PR_STORE(S, M, T, I) \ argument
138 ck_pr_md_store_##S(M *target, T v) \
161 #define CK_PR_STORE_S(S, T, I) CK_PR_STORE(S, T, T, I) argument
162 #define CK_PR_STORE_S_64(S, T, I) CK_PR_STORE_64(S, T, T, I) argument
[all …]
/f-stack/freebsd/net80211/
H A Dieee80211_crypto_wep.c347 #define S_SWAP(a,b) do { uint8_t t = S[a]; S[a] = S[b]; S[b] = t; } while(0) in wep_encrypt()
355 uint8_t S[256]; in wep_encrypt() local
367 S[i] = i; in wep_encrypt()
392 *pos++ ^= S[(S[i] + S[j]) & 0xff]; in wep_encrypt()
419 j = (j + S[i]) & 0xff; in wep_encrypt()
421 icv[k] ^= S[(S[i] + S[j]) & 0xff]; in wep_encrypt()
430 #define S_SWAP(a,b) do { uint8_t t = S[a]; S[a] = S[b]; S[b] = t; } while(0) in wep_decrypt()
438 uint8_t S[256]; in wep_decrypt() local
450 S[i] = i; in wep_decrypt()
474 *pos ^= S[(S[i] + S[j]) & 0xff]; in wep_decrypt()
[all …]

12345678910>>...13