Home
last modified time | relevance | path

Searched refs:s1 (Results 1 – 25 of 35) sorted by relevance

12

/optee_os/core/lib/libtomcrypt/src/misc/
H A Dadler32.c24 unsigned long s1, s2; in adler32_update() local
28 s1 = ctx->s[0]; in adler32_update()
33 s1 += *input++; in adler32_update()
34 s2 += s1; in adler32_update()
38 if (s1 >= s_adler32_base) { in adler32_update()
39 s1 -= s_adler32_base; in adler32_update()
45 s1 += input[0]; in adler32_update()
46 s2 += s1; in adler32_update()
47 s1 += input[1]; in adler32_update()
48 s2 += s1; in adler32_update()
[all …]
/optee_os/lib/libutils/isoc/newlib/
H A Dstrcmp.c96 int _DEFUN(strcmp, (s1, s2), _CONST char *s1 _AND _CONST char *s2)
100 while (*s1 != '\0' && *s1 == *s2) {
101 s1++;
105 return (*(unsigned char *)s1) - (*(unsigned char *)s2);
111 if (!UNALIGNED(s1, s2)) {
115 a1 = (unsigned long *)s1;
133 s1 = (char *)a1;
137 while (*s1 != '\0' && *s1 == *s2) {
138 s1++;
141 return (*(unsigned char *)s1) - (*(unsigned char *)s2);
H A Dstrncmp.c96 _DEFUN (strncmp, (s1, s2, n),
97 _CONST char *s1 _AND
105 while (n-- != 0 && *s1 == *s2)
107 if (n == 0 || *s1 == '\0')
109 s1++;
113 return (*(unsigned char *) s1) - (*(unsigned char *) s2);
122 if (!UNALIGNED (s1, s2))
125 a1 = (unsigned long*)s1;
141 s1 = (char*)a1;
145 while (n-- > 0 && *s1 == *s2)
[all …]
H A Dmemcmp.c87 unsigned char *s1 = (unsigned char *)m1; variable
91 if (*s1 != *s2)
92 return *s1 - *s2;
93 s1++;
98 unsigned char *s1 = (unsigned char *)m1;
106 if (!TOO_SMALL(n) && !UNALIGNED(s1, s2)) {
111 a1 = (unsigned long *)s1;
123 s1 = (unsigned char *)a1;
128 if (*s1 != *s2)
129 return *s1 - *s2;
[all …]
H A Dstrchr.c95 _DEFUN (strchr, (s1, i),
96 _CONST char *s1 _AND
99 _CONST unsigned char *s = (_CONST unsigned char *)s1;
/optee_os/lib/libmbedtls/mbedtls/library/
H A Dpem.c278 const unsigned char *s1, *s2, *end; in mbedtls_pem_read_buffer() local
291 s1 = (unsigned char *) strstr((const char *) data, header); in mbedtls_pem_read_buffer()
293 if (s1 == NULL) { in mbedtls_pem_read_buffer()
299 if (s2 == NULL || s2 <= s1) { in mbedtls_pem_read_buffer()
303 s1 += strlen(header); in mbedtls_pem_read_buffer()
304 if (*s1 == ' ') { in mbedtls_pem_read_buffer()
305 s1++; in mbedtls_pem_read_buffer()
307 if (*s1 == '\r') { in mbedtls_pem_read_buffer()
308 s1++; in mbedtls_pem_read_buffer()
310 if (*s1 == '\n') { in mbedtls_pem_read_buffer()
[all …]
H A Dconstant_time_impl.h274 uint64_t s1; in mbedtls_ct_uint_lt() local
282 [s1] "=&r" (s1), in mbedtls_ct_uint_lt()
290 uint32_t s1; in mbedtls_ct_uint_lt()
306 [s1] "=&l" (s1), in mbedtls_ct_uint_lt()
H A Dsha512.c404 uint64x2_t s1 = (uint64x2_t) vld1q_u8(msg + 16 * 1); in mbedtls_internal_sha512_process_many_a64_crypto() local
414 s1 = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(s1))); in mbedtls_internal_sha512_process_many_a64_crypto()
431 initial_sum = vaddq_u64(s1, vld1q_u64(&K[2])); in mbedtls_internal_sha512_process_many_a64_crypto()
481 s0 = vsha512su1q_u64(vsha512su0q_u64(s0, s1), s7, vextq_u64(s4, s5, 1)); 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()
490 initial_sum = vaddq_u64(s1, vld1q_u64(&K[t + 2])); 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()
513 s4 = vsha512su1q_u64(vsha512su0q_u64(s4, s5), s3, vextq_u64(s0, s1, 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()
/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()
38 static const char s1[] = "s1"; in simple_call() local
49 simple_call_memcmp, s1, s1, sizeof(s1)); in simple_call()
59 static TEE_Result __noinline two_level_call_memcmp2(const void *s1, in two_level_call_memcmp2() argument
62 if (!FTMN_CALLEE_DONE_MEMCMP(memcmp, s1, s2, n)) in two_level_call_memcmp2()
72 static TEE_Result __noinline two_level_call_memcmp1(const void *s1, in two_level_call_memcmp1() argument
75 return two_level_call_memcmp2(s1, s2, n); in two_level_call_memcmp1()
78 static TEE_Result __noinline two_level_call_memcmp(const void *s1, in two_level_call_memcmp() argument
86 res = two_level_call_memcmp1(s1, s2, n); in two_level_call_memcmp()
[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
289 LOAD32H(s1, pt + 4); s1 ^= rk[1]; in s_rijndael_ecb_encrypt()
299 Te1(LTC_BYTE(s1, 2)) ^ in s_rijndael_ecb_encrypt()
304 Te0(LTC_BYTE(s1, 3)) ^ in s_rijndael_ecb_encrypt()
313 Te3(LTC_BYTE(s1, 0)) ^ in s_rijndael_ecb_encrypt()
318 Te2(LTC_BYTE(s1, 1)) ^ in s_rijndael_ecb_encrypt()
324 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_rijndael_ecb_encrypt()
337 Te1(LTC_BYTE(s1, 2)) ^ in s_rijndael_ecb_encrypt()
342 Te0(LTC_BYTE(s1, 3)) ^ in s_rijndael_ecb_encrypt()
351 Te3(LTC_BYTE(s1, 0)) ^ 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
54 LOAD32H(s1, pelmac->state + 4); in s_four_rounds()
60 Te1(LTC_BYTE(s1, 2)) ^ in s_four_rounds()
64 Te0(LTC_BYTE(s1, 3)) ^ in s_four_rounds()
72 Te3(LTC_BYTE(s1, 0)); in s_four_rounds()
76 Te2(LTC_BYTE(s1, 1)) ^ in s_four_rounds()
78 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_four_rounds()
81 STORE32H(s1, pelmac->state + 4); in s_four_rounds()
/optee_os/core/include/kernel/
H A Dasan.h34 void *asan_memcpy_unchecked(void *__restrict s1, const void *__restrict s2,
55 static inline void *asan_memcpy_unchecked(void *__restrict s1, 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/arch/riscv/kernel/
H A Dthread_optee_abi_rv.S110 LDR s1, REGOFF(0)(sp)
118 lw s2, 0(s1)
119 lw s3, 4(s1)
120 lw s4, 8(s1)
H A Dthread_rv.S680 get_thread_ctx s0, s1
763 lw s1, THREAD_CORE_LOCAL_FLAGS(tp)
764 slli s1, s1, THREAD_CLF_SAVED_SHIFT
765 ori s1, s1, (THREAD_CLF_TMP | THREAD_CLF_FIQ)
766 sw s1, THREAD_CORE_LOCAL_FLAGS(tp)
782 lw s1, THREAD_CORE_LOCAL_FLAGS(tp)
783 srli s1, s1, THREAD_CLF_SAVED_SHIFT
784 ori s1, s1, THREAD_CLF_TMP
785 sw s1, THREAD_CORE_LOCAL_FLAGS(tp)
/optee_os/core/arch/arm/crypto/
H A Dsha256_armv8a_ce_a32.S39 .macro add_update, ev, s0, s1, s2, s3
40 sha256su0.32 q\s0, q\s1
41 add_only \ev, \s1
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
47 add_only \op, \ev, \rc, \s1, \dg1
H A Dsha256_armv8a_ce_a64.S43 .macro add_update, ev, rc, s0, s1, s2, s3
44 sha256su0 v\s0\().4s, v\s1\().4s
45 add_only \ev, \rc, \s1
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
53 add_only \op, \ev, \rc, \s1, \dg1
H A Dsm3_armv8a_ce_a64.S52 .macro qround, ab, s0, s1, s2, s3, s4
54 ext \s4\().16b, \s1\().16b, \s2\().16b, #12
55 ext v6.16b, \s0\().16b, \s1\().16b, #12
60 eor v10.16b, \s0\().16b, \s1\().16b
/optee_os/core/lib/zlib/
H A Dzutil.c161 int ZLIB_INTERNAL zmemcmp(s1, s2, len) in zmemcmp() argument
162 const Bytef* s1; in zmemcmp()
169 if (s1[j] != s2[j]) return 2*(s1[j] > s2[j])-1;
/optee_os/core/arch/riscv/include/kernel/
H A Dthread_arch.h76 unsigned long s1; member
140 unsigned long s1; member
/optee_os/lib/libutils/isoc/arch/riscv/
H A Dsetjmp_rv.S11 STR s1, REGOFF(1)(a0)
71 LDR s1, REGOFF(1)(a0)

12