Home
last modified time | relevance | path

Searched refs:i (Results 1 – 25 of 383) sorted by relevance

12345678910>>...16

/optee_os/core/lib/libtomcrypt/src/encauth/gcm/
H A Dgcm_gf_mult.c111 int i, j, k, u; in gcm_gf_mult() local
120 for (i = 0; i < 4; i++) { in gcm_gf_mult()
121 LOAD32H(B[M(1)][i], a + (i<<2)); in gcm_gf_mult()
122 LOAD32L(pB[i], b + (i<<2)); in gcm_gf_mult()
125 for (i = 0; i < 2; i++) { in gcm_gf_mult()
126 LOAD64H(B[M(1)][i], a + (i<<3)); in gcm_gf_mult()
127 LOAD64L(pB[i], b + (i<<3)); in gcm_gf_mult()
135 for (i = 1; i < (int)WPV; i++) { in gcm_gf_mult()
136 B[M(2)][i] = (B[M(1)][i-1] << (BPD-1)) | (B[M(1)][i] >> 1); in gcm_gf_mult()
137 B[M(4)][i] = (B[M(1)][i-1] << (BPD-2)) | (B[M(1)][i] >> 2); in gcm_gf_mult()
[all …]
/optee_os/core/lib/libtomcrypt/src/misc/pkcs5/
H A Dpkcs_5_test.c153 int i, err; in pkcs_5_test()
165 for(i=0; i < (int)(sizeof(cases_5_2) / sizeof(cases_5_2[0])); i++) { in pkcs_5_test()
167 dkLen = cases_5_2[i].dkLen; in pkcs_5_test()
168 if((err = pkcs_5_alg2((unsigned char*)cases_5_2[i].P, cases_5_2[i].P_len, in pkcs_5_test()
169 (unsigned char*)cases_5_2[i].S, cases_5_2[i].S_len, in pkcs_5_test()
170 cases_5_2[i].c, hash, in pkcs_5_test()
174 printf("\npkcs_5_alg2() #%d: Failed/1 (%s)\n", i, error_to_string(err)); in pkcs_5_test()
178 … else if (compare_testvector(DK, dkLen, cases_5_2[i].DK, cases_5_2[i].dkLen, "PKCS#5_2", i)) { in pkcs_5_test()
184 for(i=0; i < (int)(sizeof(cases_5_1) / sizeof(case_item)); i++, tested++) { in pkcs_5_test()
185 dkLen = cases_5_1[i].dkLen; in pkcs_5_test()
[all …]
/optee_os/core/crypto/
H A Dsm4.c19 #define GET_UINT32_BE(n, b, i) \ argument
21 (n) = ((uint32_t)(b)[(i)] << 24) | \
22 ((uint32_t)(b)[(i) + 1] << 16) | \
23 ((uint32_t)(b)[(i) + 2] << 8) | \
24 ((uint32_t)(b)[(i) + 3]); \
27 #define PUT_UINT32_BE(n, b, i) \ argument
29 (b)[(i)] = (uint8_t)((n) >> 24); \
30 (b)[(i) + 1] = (uint8_t)((n) >> 16); \
31 (b)[(i) + 2] = (uint8_t)((n) >> 8); \
32 (b)[(i) + 3] = (uint8_t)((n)); \
[all …]
/optee_os/lib/libutils/isoc/newlib/
H A Dstr-two-way.h233 size_t i; /* Index into current byte of NEEDLE. */ in two_way_short_needle() local
255 i = MAX (suffix, memory); in two_way_short_needle()
256 while (i < needle_len && (CANON_ELEMENT (needle[i]) in two_way_short_needle()
257 == CANON_ELEMENT (haystack[i + j]))) in two_way_short_needle()
258 ++i; in two_way_short_needle()
259 if (needle_len <= i) in two_way_short_needle()
262 i = suffix - 1; in two_way_short_needle()
263 while (memory < i + 1 && (CANON_ELEMENT (needle[i]) in two_way_short_needle()
264 == CANON_ELEMENT (haystack[i + j]))) in two_way_short_needle()
265 --i; in two_way_short_needle()
[all …]
/optee_os/core/lib/libtomcrypt/src/pk/ec25519/
H A Dtweetnacl.c7 #define FOR(i,n) for (i = 0;i < n;++i) argument
30 int i; in vn() local
32 FOR(i,n) d |= x[i]^y[i]; in vn()
43 int i; in set25519() local
44 FOR(i,16) r[i]=a[i]; in set25519()
49 int i; in car25519() local
51 FOR(i,16) { in car25519()
52 o[i]+=(1LL<<16); in car25519()
53 c=o[i]>>16; in car25519()
54 o[(i+1)*(i<15)]+=c-1+37*(c-1)*(i==15); in car25519()
[all …]
/optee_os/core/lib/libtomcrypt/src/stream/salsa20/
H A Dsalsa20_crypt.c23 int i; in s_salsa20_block() local
25 for (i = rounds; i > 0; i -= 2) { in s_salsa20_block()
35 for (i = 0; i < 16; ++i) { in s_salsa20_block()
36 x[i] += input[i]; in s_salsa20_block()
37 STORE32L(x[i], output + 4 * i); in s_salsa20_block()
52 unsigned long i, j; in salsa20_crypt() local
63 for (i = 0; i < j; ++i, st->ksleft--) out[i] = in[i] ^ st->kstream[64 - st->ksleft]; in salsa20_crypt()
74 for (i = 0; i < inlen; ++i) out[i] = in[i] ^ buf[i]; in salsa20_crypt()
76 for (i = inlen; i < 64; ++i) st->kstream[i] = buf[i]; in salsa20_crypt()
79 for (i = 0; i < 64; ++i) out[i] = in[i] ^ buf[i]; in salsa20_crypt()
/optee_os/core/lib/libtomcrypt/src/stream/chacha/
H A Dchacha_crypt.c22 int i; in s_chacha_block() local
24 for (i = rounds; i > 0; i -= 2) { in s_chacha_block()
34 for (i = 0; i < 16; ++i) { in s_chacha_block()
35 x[i] += input[i]; in s_chacha_block()
36 STORE32L(x[i], output + 4 * i); in s_chacha_block()
51 unsigned long i, j; in chacha_crypt() local
62 for (i = 0; i < j; ++i, st->ksleft--) out[i] = in[i] ^ st->kstream[64 - st->ksleft]; in chacha_crypt()
79 for (i = 0; i < inlen; ++i) out[i] = in[i] ^ buf[i]; in chacha_crypt()
81 for (i = inlen; i < 64; ++i) st->kstream[i] = buf[i]; in chacha_crypt()
84 for (i = 0; i < 64; ++i) out[i] = in[i] ^ buf[i]; in chacha_crypt()
/optee_os/core/drivers/imx/dcp/
H A Ddcp_utils.c43 unsigned int i = 0; in dcp_left_shift_buffer() local
47 for (i = 0; i < buffer_size; i++) { in dcp_left_shift_buffer()
49 result[buffer_size - 1 - i] = in dcp_left_shift_buffer()
50 input[buffer_size - 1 - i] << 1 | overflow; in dcp_left_shift_buffer()
52 overflow = input[buffer_size - 1 - i] >> 7; in dcp_left_shift_buffer()
69 unsigned int i = 0; in dcp_reverse() local
71 for (i = 0; i < size; i++) in dcp_reverse()
72 out[i] = in[size - 1 - i]; in dcp_reverse()
77 unsigned int i = 0; in dcp_xor() local
79 for (i = 0; i < size; i++) in dcp_xor()
[all …]
/optee_os/lib/libmbedtls/mbedtls/library/
H A Dconstant_time.c72 size_t i = 0; in mbedtls_ct_memcmp() local
84 for (; (i + 4) <= n; i += 4) { in mbedtls_ct_memcmp()
85 uint32_t x = mbedtls_get_unaligned_volatile_uint32(A + i); in mbedtls_ct_memcmp()
86 uint32_t y = mbedtls_get_unaligned_volatile_uint32(B + i); in mbedtls_ct_memcmp()
91 for (; i < n; i++) { in mbedtls_ct_memcmp()
95 unsigned char x = A[i], y = B[i]; in mbedtls_ct_memcmp()
134 for (size_t i = 0; i < n; i++) { in mbedtls_ct_memcmp_partial() local
135 unsigned char x = A[i], y = B[i]; in mbedtls_ct_memcmp_partial()
137 mbedtls_ct_condition_t valid = mbedtls_ct_bool_and(mbedtls_ct_uint_ge(i, skip_head), in mbedtls_ct_memcmp_partial()
138 mbedtls_ct_uint_lt(i, valid_end)); in mbedtls_ct_memcmp_partial()
[all …]
H A Dbignum_core.c55 int i; in mbedtls_mpi_core_bitlen() local
58 for (i = ((int) A_limbs) - 1; i >= 0; i--) { in mbedtls_mpi_core_bitlen()
59 if (A[i] != 0) { in mbedtls_mpi_core_bitlen()
60 j = biL - mbedtls_mpi_core_clz(A[i]); in mbedtls_mpi_core_bitlen()
61 return (i * biL) + j; in mbedtls_mpi_core_bitlen()
123 for (size_t i = 1; i < A_limbs; i++) { in mbedtls_mpi_core_uint_le_mpi() local
124 msll_mask = mbedtls_ct_bool_or(msll_mask, mbedtls_ct_bool(A[i])); in mbedtls_mpi_core_uint_le_mpi()
138 for (size_t i = limbs; i > 0; i--) { in mbedtls_mpi_core_lt_ct() local
146 cond = mbedtls_ct_uint_lt(B[i - 1], A[i - 1]); in mbedtls_mpi_core_lt_ct()
155 cond = mbedtls_ct_uint_lt(A[i - 1], B[i - 1]); in mbedtls_mpi_core_lt_ct()
[all …]
H A Daria.c325 uint8_t i, j; in aria_rot128() local
333 for (i = 0; i < 4; i++) { in aria_rot128()
339 r[i] = a[i] ^ t; // store in aria_rot128()
358 int i; in mbedtls_aria_setkey_enc() local
381 i = (keybits - 128) >> 6; // index: 0, 1, 2 in mbedtls_aria_setkey_enc()
382 ctx->nr = 12 + 2 * i; // no. rounds: 12, 14, 16 in mbedtls_aria_setkey_enc()
384 aria_fo_xor(w[1], w[0], rc[i], w[1]); // W1 = FO(W0, CK1) ^ KR in mbedtls_aria_setkey_enc()
385 i = i < 2 ? i + 1 : 0; in mbedtls_aria_setkey_enc()
386 aria_fe_xor(w[2], w[1], rc[i], w[0]); // W2 = FE(W1, CK2) ^ W0 in mbedtls_aria_setkey_enc()
387 i = i < 2 ? i + 1 : 0; in mbedtls_aria_setkey_enc()
[all …]
H A Ddes.c314 int i; in mbedtls_des_key_set_parity() local
316 for (i = 0; i < MBEDTLS_DES_KEY_SIZE; i++) { in mbedtls_des_key_set_parity()
317 key[i] = odd_parity_table[key[i] / 2]; in mbedtls_des_key_set_parity()
326 int i; in mbedtls_des_key_check_key_parity() local
328 for (i = 0; i < MBEDTLS_DES_KEY_SIZE; i++) { in mbedtls_des_key_check_key_parity()
329 if (key[i] != odd_parity_table[key[i] / 2]) { in mbedtls_des_key_check_key_parity()
383 int i; in mbedtls_des_key_check_weak() local
385 for (i = 0; i < WEAK_KEY_COUNT; i++) { in mbedtls_des_key_check_weak()
386 if (memcmp(weak_key_table[i], key, MBEDTLS_DES_KEY_SIZE) == 0) { in mbedtls_des_key_check_weak()
397 int i; in mbedtls_des_setkey() local
[all …]
H A Dcamellia.c239 for (i = 1; i <= 4; i++) \
240 if (shifts[(INDEX)][(OFFSET)][i -1]) \
241 ROTL(TK + i * 4, TK, (15 * i) % 32); \
243 for (i = 0; i < 20; i++) \
244 if (indexes[(INDEX)][(OFFSET)][i] != -1) { \
245 RK[indexes[(INDEX)][(OFFSET)][i]] = TK[i]; \
296 size_t i; in mbedtls_camellia_setkey_enc() local
315 for (i = 0; i < keybits / 8; ++i) { in mbedtls_camellia_setkey_enc()
316 t[i] = key[i]; in mbedtls_camellia_setkey_enc()
320 for (i = 0; i < 8; i++) { in mbedtls_camellia_setkey_enc()
[all …]
H A Dcommon.h201 size_t i = 0; in mbedtls_xor() local
206 for (; (i + 16) <= n; i += 16) { in mbedtls_xor()
207 uint8x16_t v1 = vld1q_u8(a + i); in mbedtls_xor()
208 uint8x16_t v2 = vld1q_u8(b + i); in mbedtls_xor()
210 vst1q_u8(r + i, x); in mbedtls_xor()
225 for (; (i + 8) <= n; i += 8) { in mbedtls_xor()
226 uint64_t x = mbedtls_get_unaligned_uint64(a + i) ^ mbedtls_get_unaligned_uint64(b + i); in mbedtls_xor()
227 mbedtls_put_unaligned_uint64(r + i, x); in mbedtls_xor()
235 for (; (i + 4) <= n; i += 4) { in mbedtls_xor()
236 uint32_t x = mbedtls_get_unaligned_uint32(a + i) ^ mbedtls_get_unaligned_uint32(b + i); in mbedtls_xor()
[all …]
/optee_os/core/lib/libtomcrypt/src/hashes/
H A Dsha1.c42 ulong32 a,b,c,d,e,W[80],i; in ss_sha1_compress() local
48 for (i = 0; i < 16; i++) { in ss_sha1_compress()
49 LOAD32H(W[i], buf + (4*i)); in ss_sha1_compress()
60 for (i = 16; i < 80; i++) { in ss_sha1_compress()
61 W[i] = ROL(W[i-3] ^ W[i-8] ^ W[i-14] ^ W[i-16], 1); in ss_sha1_compress()
66 … #define FF0(a,b,c,d,e,i) e = (ROLc(a, 5) + F0(b,c,d) + e + W[i] + 0x5a827999UL); b = ROLc(b, 30); in ss_sha1_compress() argument
67 … #define FF1(a,b,c,d,e,i) e = (ROLc(a, 5) + F1(b,c,d) + e + W[i] + 0x6ed9eba1UL); b = ROLc(b, 30); in ss_sha1_compress() argument
68 … #define FF2(a,b,c,d,e,i) e = (ROLc(a, 5) + F2(b,c,d) + e + W[i] + 0x8f1bbcdcUL); b = ROLc(b, 30); in ss_sha1_compress() argument
69 … #define FF3(a,b,c,d,e,i) e = (ROLc(a, 5) + F3(b,c,d) + e + W[i] + 0xca62c1d6UL); b = ROLc(b, 30); in ss_sha1_compress() argument
73 for (i = 0; i < 20; ) { in ss_sha1_compress()
[all …]
H A Dblake2s.c163 int i; in s_blake2s_init0() local
166 for (i = 0; i < 8; ++i) { in s_blake2s_init0()
167 md->blake2s.h[i] = blake2s_IV[i]; in s_blake2s_init0()
176 unsigned long i; in s_blake2s_init_param() local
181 for (i = 0; i < 8; ++i) { in s_blake2s_init_param()
183 LOAD32L(tmp, P + i * 4); in s_blake2s_init_param()
184 md->blake2s.h[i] ^= tmp; in s_blake2s_init_param()
270 #define G(r, i, a, b, c, d) … argument
272 …a = a + b + m[blake2s_sigma[r][2 * i + 0]]; …
276 …a = a + b + m[blake2s_sigma[r][2 * i + 1]]; …
[all …]
H A Dblake2b.c171 unsigned long i; in s_blake2b_init0() local
174 for (i = 0; i < 8; ++i) { in s_blake2b_init0()
175 md->blake2b.h[i] = blake2b_IV[i]; in s_blake2b_init0()
182 unsigned long i; in s_blake2b_init_param() local
187 for (i = 0; i < 8; ++i) { in s_blake2b_init_param()
189 LOAD64L(tmp, P + i * 8); in s_blake2b_init_param()
190 md->blake2b.h[i] ^= tmp; in s_blake2b_init_param()
277 #define G(r, i, a, b, c, d) … argument
279 …a = a + b + m[blake2b_sigma[r][2 * i + 0]]; …
283 …a = a + b + m[blake2b_sigma[r][2 * i + 1]]; …
[all …]
H A Dsha3.c159 int i, j, round; in s_keccakf() local
164 for(i = 0; i < 5; i++) { in s_keccakf()
165 bc[i] = s[i] ^ s[i + 5] ^ s[i + 10] ^ s[i + 15] ^ s[i + 20]; in s_keccakf()
167 for(i = 0; i < 5; i++) { in s_keccakf()
168 t = bc[(i + 4) % 5] ^ ROL64(bc[(i + 1) % 5], 1); in s_keccakf()
170 s[j + i] ^= t; in s_keccakf()
175 for(i = 0; i < 24; i++) { in s_keccakf()
176 j = s_keccakf_piln[i]; in s_keccakf()
178 s[j] = ROL64(t, s_keccakf_rotc[i]); in s_keccakf()
183 for(i = 0; i < 5; i++) { in s_keccakf()
[all …]
/optee_os/core/lib/libtomcrypt/src/ciphers/
H A Didea.c55 unsigned i; in s_mul_inv() local
57 for (i = 0; i < 15; i++) { in s_mul_inv()
71 int i, j; in s_setup_key() local
76 for (i = 0; i < 8; i++) { in s_setup_key()
77 LOAD16(e_key[i], key + 2 * i); in s_setup_key()
79 for (; i < LTC_IDEA_KEYLEN; i++) { in s_setup_key()
80 j = (i - i % 8) - 8; in s_setup_key()
81 e_key[i] = LOW16((e_key[j+(i+1)%8] << 9) | (e_key[j+(i+2)%8] >> 7)); in s_setup_key()
85 for (i = 0; i < LTC_IDEA_ROUNDS; i++) { in s_setup_key()
86 d_key[i*6+0] = s_mul_inv(e_key[(LTC_IDEA_ROUNDS-i)*6+0]); in s_setup_key()
[all …]
H A Drc2.c68 int i; in rc2_setup_ex() local
84 for (i = 0; i < keylen; i++) { in rc2_setup_ex()
85 tmp[i] = key[i] & 255; in rc2_setup_ex()
90 for (i = keylen; i < 128; i++) { in rc2_setup_ex()
91 tmp[i] = permute[(tmp[i - 1] + tmp[i - keylen]) & 255]; in rc2_setup_ex()
99 for (i = 127 - T8; i >= 0; i--) { in rc2_setup_ex()
100 tmp[i] = permute[tmp[i + 1] ^ tmp[i + T8]]; in rc2_setup_ex()
104 for (i = 0; i < 64; i++) { in rc2_setup_ex()
105 xkey[i] = (unsigned)tmp[2*i] + ((unsigned)tmp[2*i+1] << 8); in rc2_setup_ex()
152 unsigned x76, x54, x32, x10, i; in s_rc2_ecb_encrypt() local
[all …]
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/
H A Dsha512.c92 int i; in ss_sha512_compress() local
95 for (i = 0; i < 8; i++) { in ss_sha512_compress()
96 S[i] = md->sha512.state[i]; in ss_sha512_compress()
100 for (i = 0; i < 16; i++) { in ss_sha512_compress()
101 LOAD64H(W[i], buf + (8*i)); in ss_sha512_compress()
105 for (i = 16; i < 80; i++) { in ss_sha512_compress()
106 W[i] = Gamma1(W[i - 2]) + W[i - 7] + Gamma0(W[i - 15]) + W[i - 16]; in ss_sha512_compress()
111 for (i = 0; i < 80; i++) { in ss_sha512_compress()
112 t0 = S[7] + Sigma1(S[4]) + Ch(S[4], S[5], S[6]) + K[i] + W[i]; in ss_sha512_compress()
124 #define RND(a,b,c,d,e,f,g,h,i) \ in ss_sha512_compress() argument
[all …]
/optee_os/core/drivers/
H A Dstm32_exti.c145 unsigned int i = stm32_exti_get_bank(exti_line); in stm32_exti_event_is_configurable() local
148 return exti->trg[i] & mask; in stm32_exti_event_is_configurable()
154 unsigned int i = stm32_exti_get_bank(exti_line); in stm32_exti_set_type() local
180 io_mask32(exti->base + _EXTI_RTSR(i), r_trig, mask); in stm32_exti_set_type()
181 io_mask32(exti->base + _EXTI_FTSR(i), f_trig, mask); in stm32_exti_set_type()
188 unsigned int i = stm32_exti_get_bank(exti_line); in stm32_exti_mask() local
194 io_clrbits32(exti->base + _EXTI_C1IMR(i), mask); in stm32_exti_mask()
195 exti->mask_cache[i] &= ~mask; in stm32_exti_mask()
203 unsigned int i = stm32_exti_get_bank(exti_line); in stm32_exti_unmask() local
209 io_setbits32(exti->base + _EXTI_C1IMR(i), mask); in stm32_exti_unmask()
[all …]
/optee_os/core/lib/libtomcrypt/src/misc/hkdf/
H A Dhkdf_test.c33 int i; in hkdf_test()
254 for(i=0; i < (int)(sizeof(cases) / sizeof(cases[0])); i++) { in hkdf_test()
255 int hash = find_hash(cases[i].Hash); in hkdf_test()
258 if((err = hkdf(hash, cases[i].salt, cases[i].salt_l, in hkdf_test()
259 cases[i].info, cases[i].info_l, in hkdf_test()
260 cases[i].IKM, cases[i].IKM_l, in hkdf_test()
261 OKM, cases[i].OKM_l)) != CRYPT_OK) { in hkdf_test()
263 printf("LTC_HKDF-%s test #%d, %s\n", cases[i].Hash, i, error_to_string(err)); in hkdf_test()
268 …if(compare_testvector(OKM, cases[i].OKM_l, cases[i].OKM, (size_t)cases[i].OKM_l, "HKDF", cases[i].… in hkdf_test()
/optee_os/core/drivers/clk/sam/
H A Dat91_pmc.c23 unsigned int i = 0; in pmc_clk_get_by_id() local
25 for (i = 0; i < nclk; i++) { in pmc_clk_get_by_id()
26 if (clks[i].clk && clks[i].id == id) in pmc_clk_get_by_id()
27 return clks[i].clk; in pmc_clk_get_by_id()
36 unsigned int i = 0; in pmc_clk_get_by_name() local
38 for (i = 0; i < nclk; i++) in pmc_clk_get_by_name()
39 if (clks[i].clk && strcmp(clks[i].clk->name, name) == 0) in pmc_clk_get_by_name()
40 return clks[i].clk; in pmc_clk_get_by_name()
155 int i = 0; in pmc_register_id() local
157 for (i = 0; i < PMC_MAX_IDS; i++) { in pmc_register_id()
[all …]
/optee_os/core/drivers/firewall/
H A Dstm32_risab.c190 unsigned int i = 0; in set_block_seccfgr() local
194 for (i = subr_cfg->first_page; i <= last_page; i++) in set_block_seccfgr()
195 io_clrsetbits32(base + _RISAB_PGy_SECCFGR(i), in set_block_seccfgr()
203 unsigned int i = 0; in set_block_dprivcfgr() local
207 for (i = subr_cfg->first_page; i <= last_page; i++) in set_block_dprivcfgr()
208 io_clrsetbits32(base + _RISAB_PGy_PRIVCFGR(i), in set_block_dprivcfgr()
217 unsigned int i = 0; in set_cidcfgr() local
221 for (i = subr_cfg->first_page; i <= last_page; i++) { in set_cidcfgr()
227 io_clrsetbits32(base + _RISAB_PGy_CIDCFGR(i), in set_cidcfgr()
237 unsigned int i = 0; in set_read_conf() local
[all …]

12345678910>>...16