| /optee_os/core/lib/libtomcrypt/src/ciphers/aes/ |
| H A D | aes.c | 269 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_rijndael_ecb_encrypt() local
291 LOAD32H(s3, pt + 12); s3 ^= rk[3]; in s_rijndael_ecb_encrypt()
301 Te3(LTC_BYTE(s3, 0)) ^ in s_rijndael_ecb_encrypt()
306 Te2(LTC_BYTE(s3, 1)) ^ in s_rijndael_ecb_encrypt()
311 Te1(LTC_BYTE(s3, 2)) ^ in s_rijndael_ecb_encrypt()
316 Te0(LTC_BYTE(s3, 3)) ^ in s_rijndael_ecb_encrypt()
324 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_rijndael_ecb_encrypt()
339 Te3(LTC_BYTE(s3, 0)) ^ in s_rijndael_ecb_encrypt()
344 Te2(LTC_BYTE(s3, 1)) ^ in s_rijndael_ecb_encrypt()
349 Te1(LTC_BYTE(s3, 2)) ^ in s_rijndael_ecb_encrypt()
[all …]
|
| /optee_os/core/lib/libtomcrypt/src/mac/pelican/ |
| H A D | pelican.c | 50 ulong32 s0, s1, s2, s3, t0, t1, t2, t3; in s_four_rounds() local
56 LOAD32H(s3, pelmac->state + 12); in s_four_rounds()
62 Te3(LTC_BYTE(s3, 0)); in s_four_rounds()
66 Te2(LTC_BYTE(s3, 1)) ^ in s_four_rounds()
70 Te1(LTC_BYTE(s3, 2)) ^ in s_four_rounds()
74 Te0(LTC_BYTE(s3, 3)) ^ in s_four_rounds()
78 s0 = t0; s1 = t1; s2 = t2; s3 = t3; in s_four_rounds()
83 STORE32H(s3, pelmac->state + 12); in s_four_rounds()
|
| /optee_os/core/lib/libtomcrypt/src/mac/poly1305/ |
| H A D | poly1305.c | 18 ulong32 s1,s2,s3,s4; in s_poly1305_block() local
32 s3 = r3 * 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 …d1 = ((ulong64)h0 * r1) + ((ulong64)h1 * r0) + ((ulong64)h2 * s4) + ((ulong64)h3 * s3) + ((ulong64… in s_poly1305_block()
52 …ong64)h0 * r2) + ((ulong64)h1 * r1) + ((ulong64)h2 * r0) + ((ulong64)h3 * s4) + ((ulong64)h4 * s3); in s_poly1305_block()
|
| /optee_os/core/arch/arm/crypto/ |
| H A D | sha256_armv8a_ce_a32.S | 39 .macro add_update, ev, s0, s1, s2, s3 argument
42 sha256su1.32 q\s0, q\s2, q\s3
|
| H A D | sha1_armv8a_ce_a32.S | 45 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
48 sha1su1.32 q\s0, q\s3
|
| H A D | sm3_armv8a_ce_a64.S | 52 .macro qround, ab, s0, s1, s2, s3, s4
56 ext v7.16b, \s2\().16b, \s3\().16b, #8
57 sm3partw1 \s4\().4s, \s0\().4s, \s3\().4s
|
| H A D | sha256_armv8a_ce_a64.S | 43 .macro add_update, ev, rc, s0, s1, s2, s3 argument
46 sha256su1 v\s0\().4s, v\s2\().4s, v\s3\().4s
|
| H A D | sha1_armv8a_ce_a64.S | 51 .macro add_update, op, ev, rc, s0, s1, s2, s3, dg1
54 sha1su1 v\s0\().4s, v\s3\().4s
|
| H A D | sm4_armv8a_aese_a64.S | 252 .macro transpose_4x4, s0, s1, s2, s3 argument
254 zip1 TMP1.4s, \s2\().4s, \s3\().4s
256 zip2 TMP3.4s, \s2\().4s, \s3\().4s
260 zip2 \s3\().2d, TMP2.2d, TMP3.2d
263 .macro rotate_clockwise_90, s0, s1, s2, s3 argument
266 zip1 TMP2.4s, \s3\().4s, \s2\().4s
267 zip2 TMP3.4s, \s3\().4s, \s2\().4s
271 zip2 \s3\().2d, TMP3.2d, TMP1.2d
275 .macro round_4x, s0, s1, s2, s3, k
277 eor TMP1.16b, \s2\().16b, \s3\().16b
[all …]
|
| /optee_os/core/arch/riscv/include/kernel/ |
| H A D | thread_arch.h | 86 unsigned long s3; member
150 unsigned long s3; member
|
| /optee_os/lib/libutils/isoc/arch/riscv/ |
| H A D | setjmp_rv.S | 13 STR s3, REGOFF(3)(a0)
73 LDR s3, REGOFF(3)(a0)
|
| /optee_os/lib/libmbedtls/mbedtls/library/ |
| H A D | sha512.c | 406 uint64x2_t s3 = (uint64x2_t) vld1q_u8(msg + 16 * 3); in mbedtls_internal_sha512_process_many_a64_crypto() local
416 s3 = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(s3))); in mbedtls_internal_sha512_process_many_a64_crypto()
445 initial_sum = vaddq_u64(s3, vld1q_u64(&K[6])); 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()
505 s3 = vsha512su1q_u64(vsha512su0q_u64(s3, s4), s2, vextq_u64(s7, s0, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
506 initial_sum = vaddq_u64(s3, vld1q_u64(&K[t + 6])); 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()
529 s6 = vsha512su1q_u64(vsha512su0q_u64(s6, s7), s5, vextq_u64(s2, s3, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
537 s7 = vsha512su1q_u64(vsha512su0q_u64(s7, s0), s6, vextq_u64(s3, s4, 1)); in mbedtls_internal_sha512_process_many_a64_crypto()
|
| /optee_os/core/arch/riscv/kernel/ |
| H A D | thread_optee_abi_rv.S | 119 lw s3, 4(s1)
128 mv a2, s3 /* rv[1] */
|
| H A D | entry.S | 339 mv s3, a0
340 sw zero, THREAD_CORE_LOCAL_FLAGS(s3)
350 sw a0, THREAD_CORE_LOCAL_FLAGS(s3)
|
| H A D | abort.c | 118 ai->regs->s2, ai->regs->s3); in __print_abort_info()
|