| /optee_os/core/drivers/crypto/caam/utils/ |
| H A D | utils_sgt_v1.c | 22 SGT_TRACE("SGT[%d]->ptr_ms = %" PRIx32, idx, sgt->sgt[idx].v1.ptr_ms); in sgt_entry_trace()
23 SGT_TRACE("SGT[%d]->ptr_ls = %" PRIx32, idx, sgt->sgt[idx].v1.ptr_ls); in sgt_entry_trace()
25 sgt->sgt[idx].v1.len_f_e); in sgt_entry_trace()
26 SGT_TRACE("SGT[%d]->offset = %" PRIx32, idx, sgt->sgt[idx].v1.offset); in sgt_entry_trace()
33 len_f_e = caam_read_val32(&sgt->v1.len_f_e); in sgt_entry_offset()
38 caam_write_val32(&sgt->v1.len_f_e, len_f_e); in sgt_entry_offset()
39 caam_write_val32(&sgt->v1.offset, offset); in sgt_entry_offset()
47 caam_write_val32(&sgt->v1.ptr_ls, paddr); in caam_sgt_set_entry()
49 caam_write_val32(&sgt->v1.ptr_ms, paddr >> 32); in caam_sgt_set_entry()
51 caam_write_val32(&sgt->v1.ptr_ms, 0); in caam_sgt_set_entry()
[all …]
|
| /optee_os/core/arch/arm/crypto/ |
| H A D | aes_modes_armv8a_ce_a64.S | 152 encrypt_block2x v0, v1, w3, x2, x6, w7
157 decrypt_block2x v0, v1, w3, x2, x6, w7
164 encrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
169 decrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
198 encrypt_block2x v0, v1, w3, x2, x6, w7
202 decrypt_block2x v0, v1, w3, x2, x6, w7
206 encrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
210 decrypt_block4x v0, v1, v2, v3, w3, x2, x6, w7
220 dup v1.4s, w0
222 aese v0.16b, v1.16b
[all …]
|
| H A D | sm3_armv8a_ce_a64.S | 95 rev32 v1.16b, v1.16b
101 qround a, v0, v1, v2, v3, v4
102 qround a, v1, v2, v3, v4, v0
103 qround a, v2, v3, v4, v0, v1
104 qround a, v3, v4, v0, v1, v2
108 qround b, v4, v0, v1, v2, v3
109 qround b, v0, v1, v2, v3, v4
110 qround b, v1, v2, v3, v4, v0
111 qround b, v2, v3, v4, v0, v1
112 qround b, v3, v4, v0, v1, v2
[all …]
|
| H A D | sha3_armv8a_ce_a64.S | 64 eor v1.8b, v1.8b, v26.8b
129 eor3 v26.16b, v1.16b, v6.16b, v11.16b
146 xar v29.2d, v1.2d, v25.2d, (64 - 1)
147 xar v1.2d, v6.2d, v25.2d, (64 - 44)
198 bcax v4.16b, v28.16b, v1.16b, v0.16b
199 bcax v0.16b, v0.16b, v2.16b, v1.16b
200 bcax v1.16b, v1.16b, v27.16b, v2.16b
|
| H A D | sha512_armv8a_ce_a64.S | 131 mov v1.16b, v9.16b
191 add v9.2d, v9.2d, v1.2d
|
| /optee_os/lib/libutils/isoc/arch/arm/ |
| H A D | arm32_aeabi_ldivmod.c | 60 unsigned long long v1; member
68 unsigned long long denominator = asm_ulqr->v1; in __ul_divmod()
74 asm_ulqr->v1 = qr.r; in __ul_divmod()
79 long long v1; member
87 long long denominator = asm_lqr->v1; in __l_divmod()
103 asm_lqr->v1 = qr.r; in __l_divmod()
|
| H A D | setjmp_a32.S | 207 stmea a1!, { v1-v7, fp, ip, lr }
209 stmea a1!, { v1-v7, fp, ip}
270 ldmfd a1!, { v1-v7, fp, ip, lr }
273 ldmfd a1!, { v1-v7, fp, ip }
|
| /optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/ |
| H A D | primitiveTypes.h | 71 #define INIT_UINTM4( v3, v2, v1, v0 ) { v0, v1, v2, v3 } argument
82 #define INIT_UINTM4( v3, v2, v1, v0 ) { v3, v2, v1, v0 } argument
|
| /optee_os/core/lib/libtomcrypt/src/ciphers/ |
| H A D | tea.c | 90 ulong32 v0, v1, sum = SUM; in tea_ecb_decrypt() local
99 LOAD32H(v1, &ct[4]); in tea_ecb_decrypt()
102 v1 -= ((v0 << 4) + skey->tea.k[2]) ^ (v0 + sum) ^ ((v0 >> 5) + skey->tea.k[3]); in tea_ecb_decrypt()
103 v0 -= ((v1 << 4) + skey->tea.k[0]) ^ (v1 + sum) ^ ((v1 >> 5) + skey->tea.k[1]); in tea_ecb_decrypt()
108 STORE32H(v1, &pt[4]); in tea_ecb_decrypt()
|
| /optee_os/lib/libmbedtls/mbedtls/library/ |
| H A D | bignum_core.c | 333 size_t i, v0, v1; in mbedtls_mpi_core_shift_r() local
337 v1 = count & (biL - 1); in mbedtls_mpi_core_shift_r()
339 if (v0 > limbs || (v0 == limbs && v1 > 0)) { in mbedtls_mpi_core_shift_r()
360 if (v1 > 0) { in mbedtls_mpi_core_shift_r()
362 r1 = X[i - 1] << (biL - v1); in mbedtls_mpi_core_shift_r()
363 X[i - 1] >>= v1; in mbedtls_mpi_core_shift_r()
373 size_t i, v0, v1; in mbedtls_mpi_core_shift_l() local
377 v1 = count & (biL - 1); in mbedtls_mpi_core_shift_l()
395 if (v1 > 0) { in mbedtls_mpi_core_shift_l()
397 r1 = X[i] >> (biL - v1); in mbedtls_mpi_core_shift_l()
[all …]
|
| H A D | common.h | 207 uint8x16_t v1 = vld1q_u8(a + i); in mbedtls_xor() local
209 uint8x16_t x = veorq_u8(v1, v2); in mbedtls_xor()
|
| /optee_os/core/lib/libtomcrypt/src/pk/ecc/ |
| H A D | ecc_recover_key.c | 32 void *r, *s, *v, *w, *t1, *t2, *u1, *u2, *v1, *v2, *e, *x, *y, *a_plus3; in ecc_recover_key() local
49 …if ((err = mp_init_multi(&r, &s, &v, &w, &t1, &t2, &u1, &u2, &v1, &v2, &e, &x, &y, &a_plus3, LTC_N… in ecc_recover_key()
197 …if ((err = mp_mulmod(s, w, p, v1)) != CRYPT_OK) … in ecc_recover_key()
224 …if ((err = ltc_mp.ecc_mul2add(mR, v1, mG, v2, mQ, ma, m)) != CRYPT_OK) … in ecc_recover_key()
255 mp_clear_multi(a_plus3, y, x, e, v2, v1, u2, u1, t2, t1, w, v, s, r, LTC_NULL); in ecc_recover_key()
|
| /optee_os/core/arch/arm/dts/ |
| H A D | embedded_dtb_test.dts | 5 /dts-v1/;
|
| H A D | hikey.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-ev1-scmi.dts | 5 /dts-v1/;
|
| H A D | stm32mp157a-dk1-scmi.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-dk2-scmi.dts | 6 /dts-v1/;
|
| H A D | stm32mp215f-dk.dts | 6 /dts-v1/;
|
| H A D | stm32mp157c-dhcom-pdk2.dts | 11 /dts-v1/;
|
| H A D | stm32mp157c-ed1-scmi.dts | 5 /dts-v1/;
|
| H A D | stm32mp157a-dhcor-avenger96.dts | 13 /dts-v1/;
|
| H A D | stm32mp157a-dk1.dts | 7 /dts-v1/;
|
| /optee_os/core/lib/libtomcrypt/src/stream/sosemanuk/ |
| H A D | sosemanuk.c | 654 STORE32L(u ## x1 ^ v1, st->buf + ooff + 4); \ in s_sosemanuk_internal()
672 ulong32 v0, v1, v2, v3; in s_sosemanuk_internal() local
675 STEP(01, 02, 03, 04, 05, 06, 07, 08, 09, 00, v1, u1); in s_sosemanuk_internal()
680 STEP(05, 06, 07, 08, 09, 00, 01, 02, 03, 04, v1, u1); in s_sosemanuk_internal()
685 STEP(09, 00, 01, 02, 03, 04, 05, 06, 07, 08, v1, u1); in s_sosemanuk_internal()
690 STEP(03, 04, 05, 06, 07, 08, 09, 00, 01, 02, v1, u1); in s_sosemanuk_internal()
695 STEP(07, 08, 09, 00, 01, 02, 03, 04, 05, 06, v1, u1); in s_sosemanuk_internal()
|
| /optee_os/core/arch/arm/plat-totalcompute/fdts/ |
| H A D | optee_sp_manifest.dts | 9 /dts-v1/;
|
| /optee_os/core/drivers/crypto/caam/include/ |
| H A D | caam_utils_sgt.h | 50 } v1; member
|