Home
last modified time | relevance | path

Searched refs:s2 (Results 1 – 25 of 33) sorted by relevance

12

/optee_os/core/lib/libtomcrypt/src/misc/
H A Dadler32.c24 unsigned long s1, s2; in adler32_update() local
29 s2 = ctx->s[1]; in adler32_update()
34 s2 += s1; in adler32_update()
41 s2 %= s_adler32_base; in adler32_update()
46 s2 += s1; in adler32_update()
48 s2 += s1; in adler32_update()
50 s2 += s1; in adler32_update()
52 s2 += s1; in adler32_update()
54 s2 += s1; in adler32_update()
56 s2 += s1; in adler32_update()
[all …]
/optee_os/lib/libutils/isoc/newlib/
H A Dmemcmp.c88 unsigned char *s2 = (unsigned char *)m2; variable
91 if (*s1 != *s2)
92 return *s1 - *s2;
94 s2++;
99 unsigned char *s2 = (unsigned char *)m2;
106 if (!TOO_SMALL(n) && !UNALIGNED(s1, s2)) {
112 a2 = (unsigned long *)s2;
124 s2 = (unsigned char *)a2;
128 if (*s1 != *s2)
129 return *s1 - *s2;
[all …]
H A Dstrcmp.c96 int _DEFUN(strcmp, (s1, s2), _CONST char *s1 _AND _CONST char *s2)
100 while (*s1 != '\0' && *s1 == *s2) {
102 s2++;
105 return (*(unsigned char *)s1) - (*(unsigned char *)s2);
111 if (!UNALIGNED(s1, s2)) {
116 a2 = (unsigned long *)s2;
134 s2 = (char *)a2;
137 while (*s1 != '\0' && *s1 == *s2) {
139 s2++;
141 return (*(unsigned char *)s1) - (*(unsigned char *)s2);
H A Dstrncmp.c96 _DEFUN (strncmp, (s1, s2, n),
98 _CONST char *s2 _AND
105 while (n-- != 0 && *s1 == *s2)
110 s2++;
113 return (*(unsigned char *) s1) - (*(unsigned char *) s2);
122 if (!UNALIGNED (s1, s2))
126 a2 = (unsigned long*)s2;
142 s2 = (char*)a2;
145 while (n-- > 0 && *s1 == *s2)
152 s2++;
[all …]
/optee_os/core/tests/
H A Dftmn_boot_tests.c26 static TEE_Result __noinline simple_call_memcmp(const void *s1, const void *s2, in simple_call_memcmp() argument
29 if (!FTMN_CALLEE_DONE_MEMCMP(memcmp, s1, s2, n)) in simple_call_memcmp()
60 const void *s2, size_t n) in two_level_call_memcmp2() argument
62 if (!FTMN_CALLEE_DONE_MEMCMP(memcmp, s1, s2, n)) in two_level_call_memcmp2()
73 const void *s2, size_t n) in two_level_call_memcmp1() argument
75 return two_level_call_memcmp2(s1, s2, n); in two_level_call_memcmp1()
79 const void *s2, size_t n) in two_level_call_memcmp() argument
86 res = two_level_call_memcmp1(s1, s2, n); in two_level_call_memcmp()
99 static const char s2[] = "s2"; in two_level_call() local
106 two_level_call_memcmp, s1, s2, sizeof(s1)); in two_level_call()
[all …]
/optee_os/lib/libutils/isoc/include/
H A Dstring.h17 void *memcpy(void *__restrict s1, const void *__restrict s2, size_t n);
18 void *memmove(void *s1, const void *s2, size_t n);
19 int memcmp(const void *s1, const void *s2, size_t n);
22 int strcmp(const char *s1, const char *s2);
23 int strncmp(const char *s1, const char *s2, size_t n);
H A Dstrings.h8 int bcmp(const void *s1, const void *s2, size_t n);
/optee_os/core/lib/libtomcrypt/src/ciphers/aes/
H A Daes.c269 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_rijndael_ecb_encrypt() local
290 LOAD32H(s2, pt + 8); s2 ^= rk[2]; in s_rijndael_ecb_encrypt()
300 Te2(LTC_BYTE(s2, 1)) ^ in s_rijndael_ecb_encrypt()
305 Te1(LTC_BYTE(s2, 2)) ^ in s_rijndael_ecb_encrypt()
310 Te0(LTC_BYTE(s2, 3)) ^ in s_rijndael_ecb_encrypt()
319 Te3(LTC_BYTE(s2, 0)) ^ in s_rijndael_ecb_encrypt()
324 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_rijndael_ecb_encrypt()
338 Te2(LTC_BYTE(s2, 1)) ^ in s_rijndael_ecb_encrypt()
343 Te1(LTC_BYTE(s2, 2)) ^ in s_rijndael_ecb_encrypt()
348 Te0(LTC_BYTE(s2, 3)) ^ in s_rijndael_ecb_encrypt()
[all …]
/optee_os/core/lib/libtomcrypt/src/mac/pelican/
H A Dpelican.c50 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_four_rounds() local
55 LOAD32H(s2, pelmac->state + 8); in s_four_rounds()
61 Te2(LTC_BYTE(s2, 1)) ^ in s_four_rounds()
65 Te1(LTC_BYTE(s2, 2)) ^ in s_four_rounds()
69 Te0(LTC_BYTE(s2, 3)) ^ in s_four_rounds()
77 Te3(LTC_BYTE(s2, 0)); in s_four_rounds()
78 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_four_rounds()
82 STORE32H(s2, pelmac->state + 8); in s_four_rounds()
/optee_os/lib/libmbedtls/mbedtls/library/
H A Dpem.c278 const unsigned char *s1, *s2, *end; in mbedtls_pem_read_buffer() local
297 s2 = (unsigned char *) strstr((const char *) data, footer); in mbedtls_pem_read_buffer()
299 if (s2 == NULL || s2 <= s1) { in mbedtls_pem_read_buffer()
316 end = s2; in mbedtls_pem_read_buffer()
331 if (s2 - s1 >= 22 && memcmp(s1, "Proc-Type: 4,ENCRYPTED", 22) == 0) { in mbedtls_pem_read_buffer()
347 if (s2 - s1 >= 23 && memcmp(s1, "DEK-Info: DES-EDE3-CBC,", 23) == 0) { in mbedtls_pem_read_buffer()
351 if (s2 - s1 < 16 || pem_get_iv(s1, pem_iv, 8) != 0) { in mbedtls_pem_read_buffer()
356 } else if (s2 - s1 >= 18 && memcmp(s1, "DEK-Info: DES-CBC,", 18) == 0) { in mbedtls_pem_read_buffer()
360 if (s2 - s1 < 16 || pem_get_iv(s1, pem_iv, 8) != 0) { in mbedtls_pem_read_buffer()
369 if (s2 - s1 >= 14 && memcmp(s1, "DEK-Info: AES-", 14) == 0) { in mbedtls_pem_read_buffer()
[all …]
H A Dsha512.c405 uint64x2_t s2 = (uint64x2_t) vld1q_u8(msg + 16 * 2); in mbedtls_internal_sha512_process_many_a64_crypto() local
415 s2 = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(s2))); in mbedtls_internal_sha512_process_many_a64_crypto()
438 initial_sum = vaddq_u64(s2, vld1q_u64(&K[4])); in mbedtls_internal_sha512_process_many_a64_crypto()
489 s1 = vsha512su1q_u64(vsha512su0q_u64(s1, s2), s0, vextq_u64(s5, s6, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
497 s2 = vsha512su1q_u64(vsha512su0q_u64(s2, s3), s1, vextq_u64(s6, s7, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
498 initial_sum = vaddq_u64(s2, vld1q_u64(&K[t + 4])); in mbedtls_internal_sha512_process_many_a64_crypto()
505 s3 = vsha512su1q_u64(vsha512su0q_u64(s3, s4), s2, vextq_u64(s7, s0, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
521 s5 = vsha512su1q_u64(vsha512su0q_u64(s5, s6), s4, vextq_u64(s1, s2, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
529 s6 = vsha512su1q_u64(vsha512su0q_u64(s6, s7), s5, vextq_u64(s2, s3, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
/optee_os/core/include/kernel/
H A Dasan.h34 void *asan_memcpy_unchecked(void *__restrict s1, const void *__restrict s2,
56 const void *__restrict s2, size_t n) in asan_memcpy_unchecked() argument
58 return memcpy(s1, s2, n); in asan_memcpy_unchecked()
/optee_os/lib/libutils/ext/include/
H A Dstring_ext.h28 static inline int buf_compare_ct(const void *s1, const void *s2, size_t n) in buf_compare_ct() argument
30 return consttime_memcmp(s1, s2, n); in buf_compare_ct()
/optee_os/core/lib/zlib/
H A Dzutil.c161 int ZLIB_INTERNAL zmemcmp(s1, s2, len) in zmemcmp() argument
163 const Bytef* s2;
169 if (s1[j] != s2[j]) return 2*(s1[j] > s2[j])-1;
/optee_os/core/arch/arm/crypto/
H A Dsha256_armv8a_ce_a32.S39 .macro add_update, ev, s0, s1, s2, s3
42 sha256su1.32 q\s0, q\s2, q\s3
H A Dsha1_armv8a_ce_a32.S45 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
46 sha1su0.32 q\s0, q\s1, q\s2
H A Dsm3_armv8a_ce_a64.S52 .macro qround, ab, s0, s1, s2, s3, s4
54 ext \s4\().16b, \s1\().16b, \s2\().16b, #12
56 ext v7.16b, \s2\().16b, \s3\().16b, #8
H A Dsha256_armv8a_ce_a64.S43 .macro add_update, ev, rc, s0, s1, s2, s3
46 sha256su1 v\s0\().4s, v\s2\().4s, v\s3\().4s
H A Dsha1_armv8a_ce_a64.S51 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
52 sha1su0 v\s0\().4s, v\s1\().4s, v\s2\().4s
/optee_os/scripts/
H A Dts_bin_to_c.py74 s2 = elffile.get_section(symbol.entry['st_shndx'])
75 offs = s2.header['sh_offset'] - s2.header['sh_addr']
/optee_os/core/arch/riscv/include/kernel/
H A Dthread_arch.h85 unsigned long s2; member
149 unsigned long s2; member
/optee_os/lib/libutils/isoc/arch/riscv/
H A Dsetjmp_rv.S12 STR s2, REGOFF(2)(a0)
72 LDR s2, REGOFF(2)(a0)
/optee_os/core/lib/libtomcrypt/src/mac/poly1305/
H A Dpoly1305.c18 ulong32 s1,s2,s3,s4; in s_poly1305_block() local
31 s2 = r2 * 5; in s_poly1305_block()
50 …d0 = ((ulong64)h0 * r0) + ((ulong64)h1 * s4) + ((ulong64)h2 * s3) + ((ulong64)h3 * s2) + ((ulong64… in s_poly1305_block()
51 …ong64)h0 * r1) + ((ulong64)h1 * r0) + ((ulong64)h2 * s4) + ((ulong64)h3 * s3) + ((ulong64)h4 * s2); in s_poly1305_block()
/optee_os/core/arch/riscv/kernel/
H A Dthread_optee_abi_rv.S118 lw s2, 0(s1)
127 mv a1, s2 /* rv[0] */
H A Dasm-defines.c54 DEFINE(THREAD_CTX_REG_S2, offsetof(struct thread_ctx_regs, s2));
77 DEFINE(THREAD_ABT_REG_S2, offsetof(struct thread_abort_regs, s2));

12