Home
last modified time | relevance | path

Searched refs:s4 (Results 1 – 7 of 7) sorted by relevance

/optee_os/core/arch/arm/crypto/
H A Dsm3_armv8a_ce_a64.S52 .macro qround, ab, s0, s1, s2, s3, s4 argument
53 .ifnb \s4
54 ext \s4\().16b, \s1\().16b, \s2\().16b, #12
57 sm3partw1 \s4\().4s, \s0\().4s, \s3\().4s
67 .ifnb \s4
68 sm3partw2 \s4\().4s, v7.4s, v6.4s
/optee_os/core/lib/libtomcrypt/src/mac/poly1305/
H A Dpoly1305.c18 ulong32 s1,s2,s3,s4; in s_poly1305_block() local
33 s4 = r4 * 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 …d2 = ((ulong64)h0 * r2) + ((ulong64)h1 * r1) + ((ulong64)h2 * r0) + ((ulong64)h3 * s4) + ((ulong64… in s_poly1305_block()
53 …ong64)h0 * r3) + ((ulong64)h1 * r2) + ((ulong64)h2 * r1) + ((ulong64)h3 * r0) + ((ulong64)h4 * s4); in s_poly1305_block()
/optee_os/core/arch/riscv/include/kernel/
H A Dthread_arch.h87 unsigned long s4; member
151 unsigned long s4; member
/optee_os/lib/libutils/isoc/arch/riscv/
H A Dsetjmp_rv.S14 STR s4, REGOFF(4)(a0)
74 LDR s4, REGOFF(4)(a0)
/optee_os/lib/libmbedtls/mbedtls/library/
H A Dsha512.c407 uint64x2_t s4 = (uint64x2_t) vld1q_u8(msg + 16 * 4); in mbedtls_internal_sha512_process_many_a64_crypto() local
417 s4 = vreinterpretq_u64_u8(vrev64q_u8(vreinterpretq_u8_u64(s4))); in mbedtls_internal_sha512_process_many_a64_crypto()
452 initial_sum = vaddq_u64(s4, vld1q_u64(&K[8])); 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()
505 s3 = vsha512su1q_u64(vsha512su0q_u64(s3, s4), s2, vextq_u64(s7, s0, 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()
514 initial_sum = vaddq_u64(s4, vld1q_u64(&K[t + 8])); 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()
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 Dthread_optee_abi_rv.S120 lw s4, 8(s1)
129 mv a3, s4 /* rv[2] */
H A Dabort.c119 EMSG_RAW("s4\t%016" PRIxPTR " s5\t%016" PRIxPTR, in __print_abort_info()
120 ai->regs->s4, ai->regs->s5); in __print_abort_info()