History log of /optee_os/core/ (Results 4076 – 4100 of 6456)
Revision Date Author Comments
(<<< Hide modified files)
(Show modified files >>>)
6e9e277f13-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: move sockets PTA to core/tee

The sockets pseudo-TA is architecture-independent. Move it to
core/tee and drop the pta_ prefix which is not really useful.

Signed-off-by: Jerome Forissier <jerom

core: move sockets PTA to core/tee

The sockets pseudo-TA is architecture-independent. Move it to
core/tee and drop the pta_ prefix which is not really useful.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

5843bb7513-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: move PTAs from core/arch/arm/pta to core/pta

All pseudo-TAs in core/arch/arm/pta are not architecture-
specific so move them out of the arch directory.

sdp_pta.c is renamed sdp.c since _pta i

core: move PTAs from core/arch/arm/pta to core/pta

All pseudo-TAs in core/arch/arm/pta are not architecture-
specific so move them out of the arch directory.

sdp_pta.c is renamed sdp.c since _pta is redundant.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

963051aa13-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: move test PTAs to core/pta/tests

Moves the test PTAs out of the arch-dependent tree into core/pta/tests.
File names are shortened a bit since the full paths make the purpose
clear.

Signed-off

core: move test PTAs to core/pta/tests

Moves the test PTAs out of the arch-dependent tree into core/pta/tests.
File names are shortened a bit since the full paths make the purpose
clear.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

e86a7b9213-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: prepare to move PTAs under core/pta and core/pta/tests

Most pseudo-TAs are currently under core/arch/arm/pta. This is wrong
since none of those are architecture-dependent. This patch creates
c

core: prepare to move PTAs under core/pta and core/pta/tests

Most pseudo-TAs are currently under core/arch/arm/pta. This is wrong
since none of those are architecture-dependent. This patch creates
core/pta and core/pta/tests to prepare for the following scheme:
- PTAs that implement a GP TEE API (sockets, for example) should be in
core/tee
- PTAs that implement other system services should be in /core/pta
- Test PTAs should be in core/pta/tests
- Platform-specific PTAs belong in the platform's directory
- Architecture-specific (but not platform-specific) PTAs should go
in core/arch/$(ARCH)/pta (there are none currently)

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

4b05407413-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: pta/gprof.c: remove <arm.h> include

The gprof pseudo-TA does not need <arm.h> so remove it.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@

core: pta/gprof.c: remove <arm.h> include

The gprof pseudo-TA does not need <arm.h> so remove it.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

5a913ee720-Aug-2019 Jerome Forissier <jerome@forissier.org>

Squashed commit upgrading to libtomcrypt-1.18.2-develop-20180819

Squash merging branch import/libtomcrypt-1.18.2-develop-20180819

5ecac6e9227c ("core: ltc: adapt to new version of LibTomCrypt")
54d

Squashed commit upgrading to libtomcrypt-1.18.2-develop-20180819

Squash merging branch import/libtomcrypt-1.18.2-develop-20180819

5ecac6e9227c ("core: ltc: adapt to new version of LibTomCrypt")
54d7f2f10c33 ("core: ltc: aes_modes_armv8a_ce_a64.S: get rid of literal load of addend vector")
68b1adf4c3db ("core: ltc: aes_modes_armv8a_ce_a64.S: fix incorrect assembly syntax")
b73cfbef058f ("core: ltc: make key in accel_ecb_encrypt() and accel_ecb_decrypt() const")
7160452f6698 ("core: ltc: fix 'switch case misses default'")
05313fd03df1 ("core: ltc: move AES CE files under aes/")
00ed54001f7d ("core: ltc: add custom DH key generation function dh_make_key()")
279e09ee4c7c ("core: ltc: tomcrypt_custom.h: OP-TEE thread support")
e61adb1a2203 ("core: crypto: libtomcrypt: fix LTC_CLEAN_STACK bug")
5c75c2d02f13 ("core: LTC use only _CFG_CORE_LTC_ variables")
5decfe20864a ("core: crypto: arm64 ce: update AES CBC routines")
c54b6344cc4e ("core: crypto: cleanup and fix CE accelerated AES CTR")
3f4d78d04eef ("core: crypto: arm32: add counter increment in ce_aes_ctr_encrypt()")
a85a4f88e39d ("Remove 'All rights reserved' from Linaro files")
14ec45d62762 ("Remove license notice from Linaro files")
084691667db2 ("Add SPDX license identifiers")
48de810896b8 ("LTC: add GHASH acceleration")
9f4ecf2ea898 ("arm32: AES using ARMv8-A cryptographic extensions")
a360627e4130 ("arm64: libtomcrypt: rename AES CE files")
48dab9f6464b ("arm64: libtomcrypt: move inline assembly to .S file")
7479ed2a4be9 ("ltc: bugfix find_prng()")
271db0fe9309 ("ltc: make cipher_descriptor a pointer to descriptors")
cbf6e51b6086 ("ltc: make hash_descriptor a pointer to descriptors")
6982b2b65910 ("ltc: make prng_descriptor a pointer to descriptors")
034ed64a6bb2 ("arm: Fix SHA-1 with cryptographic extensions")
468fcca20d8b ("arm64: SHA-224/SHA-256 using ARMv8-A cryptographic extensions")
a55567f8611c ("arm: update SHA-256 32-bit CE implementation to process multiple blocks")
ee62ece8ecf4 ("arm: update SHA-1 32-bit CE implementation to process multiple blocks")
4287faa43c7c ("arm64: SHA-1 using ARMv8-A cryptographic extensions")
0c6c51d33f05 ("ECC: optimize the pool of temporary variables")
f79f07210b95 ("arm64: AES XTS using ARMv8-A cryptographic extensions")
dc3e64eee4af ("arm64: AES using ARMv8-A cryptographic extensions")
fcad408195d8 ("SHA-1 ARMv8 crypto extension implementation")
e9fa8daa66ed ("SHA-256 ARMv8 crypto extension implementation")
36c11ddb0f2f ("Import LibTomCrypt v1.18.2 branch "develop" (Aug 19, 2019)")
01c7a0fe164c ("Remove LibTomCrypt")

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...


lib/libtomcrypt/aes.c
lib/libtomcrypt/cbc.c
lib/libtomcrypt/ccm.c
lib/libtomcrypt/cmac.c
lib/libtomcrypt/ctr.c
lib/libtomcrypt/dh.c
lib/libtomcrypt/dsa.c
lib/libtomcrypt/ecb.c
lib/libtomcrypt/ecc.c
lib/libtomcrypt/gcm.c
lib/libtomcrypt/hash.c
lib/libtomcrypt/hmac.c
lib/libtomcrypt/mpa_desc.c
lib/libtomcrypt/mpi_desc.c
lib/libtomcrypt/rsa.c
lib/libtomcrypt/src/ciphers/aes/aes.c
lib/libtomcrypt/src/ciphers/aes/aes_armv8a_ce.c
lib/libtomcrypt/src/ciphers/aes/aes_modes_armv8a_ce_a32.S
lib/libtomcrypt/src/ciphers/aes/aes_modes_armv8a_ce_a64.S
lib/libtomcrypt/src/ciphers/aes/aes_tab.c
lib/libtomcrypt/src/ciphers/aes/sub.mk
lib/libtomcrypt/src/ciphers/anubis.c
lib/libtomcrypt/src/ciphers/blowfish.c
lib/libtomcrypt/src/ciphers/camellia.c
lib/libtomcrypt/src/ciphers/cast5.c
lib/libtomcrypt/src/ciphers/des.c
lib/libtomcrypt/src/ciphers/idea.c
lib/libtomcrypt/src/ciphers/kasumi.c
lib/libtomcrypt/src/ciphers/khazad.c
lib/libtomcrypt/src/ciphers/kseed.c
lib/libtomcrypt/src/ciphers/multi2.c
lib/libtomcrypt/src/ciphers/noekeon.c
lib/libtomcrypt/src/ciphers/rc2.c
lib/libtomcrypt/src/ciphers/rc5.c
lib/libtomcrypt/src/ciphers/rc6.c
lib/libtomcrypt/src/ciphers/safer/safer.c
lib/libtomcrypt/src/ciphers/safer/safer_tab.c
lib/libtomcrypt/src/ciphers/safer/saferp.c
lib/libtomcrypt/src/ciphers/serpent.c
lib/libtomcrypt/src/ciphers/skipjack.c
lib/libtomcrypt/src/ciphers/sub.mk
lib/libtomcrypt/src/ciphers/twofish/twofish.c
lib/libtomcrypt/src/ciphers/twofish/twofish_tab.c
lib/libtomcrypt/src/ciphers/xtea.c
lib/libtomcrypt/src/encauth/ccm/ccm_add_aad.c
lib/libtomcrypt/src/encauth/ccm/ccm_add_nonce.c
lib/libtomcrypt/src/encauth/ccm/ccm_done.c
lib/libtomcrypt/src/encauth/ccm/ccm_init.c
lib/libtomcrypt/src/encauth/ccm/ccm_memory.c
lib/libtomcrypt/src/encauth/ccm/ccm_process.c
lib/libtomcrypt/src/encauth/ccm/ccm_reset.c
lib/libtomcrypt/src/encauth/ccm/ccm_test.c
lib/libtomcrypt/src/encauth/ccm/sub.mk
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_add_aad.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_decrypt.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_done.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_encrypt.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_init.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_memory.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_setiv.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_setiv_rfc7905.c
lib/libtomcrypt/src/encauth/chachapoly/chacha20poly1305_test.c
lib/libtomcrypt/src/encauth/eax/eax_addheader.c
lib/libtomcrypt/src/encauth/eax/eax_decrypt.c
lib/libtomcrypt/src/encauth/eax/eax_decrypt_verify_memory.c
lib/libtomcrypt/src/encauth/eax/eax_done.c
lib/libtomcrypt/src/encauth/eax/eax_encrypt.c
lib/libtomcrypt/src/encauth/eax/eax_encrypt_authenticate_memory.c
lib/libtomcrypt/src/encauth/eax/eax_init.c
lib/libtomcrypt/src/encauth/eax/eax_test.c
lib/libtomcrypt/src/encauth/gcm/gcm_add_aad.c
lib/libtomcrypt/src/encauth/gcm/gcm_add_iv.c
lib/libtomcrypt/src/encauth/gcm/gcm_done.c
lib/libtomcrypt/src/encauth/gcm/gcm_gf_mult.c
lib/libtomcrypt/src/encauth/gcm/gcm_init.c
lib/libtomcrypt/src/encauth/gcm/gcm_memory.c
lib/libtomcrypt/src/encauth/gcm/gcm_mult_h.c
lib/libtomcrypt/src/encauth/gcm/gcm_process.c
lib/libtomcrypt/src/encauth/gcm/gcm_reset.c
lib/libtomcrypt/src/encauth/gcm/gcm_test.c
lib/libtomcrypt/src/encauth/gcm/sub.mk
lib/libtomcrypt/src/encauth/ocb/ocb_decrypt.c
lib/libtomcrypt/src/encauth/ocb/ocb_decrypt_verify_memory.c
lib/libtomcrypt/src/encauth/ocb/ocb_done_decrypt.c
lib/libtomcrypt/src/encauth/ocb/ocb_done_encrypt.c
lib/libtomcrypt/src/encauth/ocb/ocb_encrypt.c
lib/libtomcrypt/src/encauth/ocb/ocb_encrypt_authenticate_memory.c
lib/libtomcrypt/src/encauth/ocb/ocb_init.c
lib/libtomcrypt/src/encauth/ocb/ocb_ntz.c
lib/libtomcrypt/src/encauth/ocb/ocb_shift_xor.c
lib/libtomcrypt/src/encauth/ocb/ocb_test.c
lib/libtomcrypt/src/encauth/ocb/s_ocb_done.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_add_aad.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_decrypt.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_decrypt_last.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_decrypt_verify_memory.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_done.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_encrypt.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_encrypt_authenticate_memory.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_encrypt_last.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_init.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_int_ntz.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_int_xor_blocks.c
lib/libtomcrypt/src/encauth/ocb3/ocb3_test.c
lib/libtomcrypt/src/hashes/blake2b.c
lib/libtomcrypt/src/hashes/blake2s.c
lib/libtomcrypt/src/hashes/chc/chc.c
lib/libtomcrypt/src/hashes/helper/hash_file.c
lib/libtomcrypt/src/hashes/helper/hash_filehandle.c
lib/libtomcrypt/src/hashes/helper/hash_memory.c
lib/libtomcrypt/src/hashes/helper/hash_memory_multi.c
lib/libtomcrypt/src/hashes/helper/sub.mk
lib/libtomcrypt/src/hashes/md2.c
lib/libtomcrypt/src/hashes/md4.c
lib/libtomcrypt/src/hashes/md5.c
lib/libtomcrypt/src/hashes/rmd128.c
lib/libtomcrypt/src/hashes/rmd160.c
lib/libtomcrypt/src/hashes/rmd256.c
lib/libtomcrypt/src/hashes/rmd320.c
lib/libtomcrypt/src/hashes/sha1.c
lib/libtomcrypt/src/hashes/sha1_armv8a_ce.c
lib/libtomcrypt/src/hashes/sha2/sha224.c
lib/libtomcrypt/src/hashes/sha2/sha256.c
lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce.c
lib/libtomcrypt/src/hashes/sha2/sha384.c
lib/libtomcrypt/src/hashes/sha2/sha512.c
lib/libtomcrypt/src/hashes/sha2/sha512_224.c
lib/libtomcrypt/src/hashes/sha2/sha512_256.c
lib/libtomcrypt/src/hashes/sha3.c
lib/libtomcrypt/src/hashes/sha3_test.c
lib/libtomcrypt/src/hashes/tiger.c
lib/libtomcrypt/src/hashes/whirl/whirl.c
lib/libtomcrypt/src/hashes/whirl/whirltab.c
lib/libtomcrypt/src/headers/tomcrypt.h
lib/libtomcrypt/src/headers/tomcrypt_argchk.h
lib/libtomcrypt/src/headers/tomcrypt_arm_neon.h
lib/libtomcrypt/src/headers/tomcrypt_cfg.h
lib/libtomcrypt/src/headers/tomcrypt_cipher.h
lib/libtomcrypt/src/headers/tomcrypt_custom.h
lib/libtomcrypt/src/headers/tomcrypt_hash.h
lib/libtomcrypt/src/headers/tomcrypt_mac.h
lib/libtomcrypt/src/headers/tomcrypt_macros.h
lib/libtomcrypt/src/headers/tomcrypt_math.h
lib/libtomcrypt/src/headers/tomcrypt_misc.h
lib/libtomcrypt/src/headers/tomcrypt_pk.h
lib/libtomcrypt/src/headers/tomcrypt_pkcs.h
lib/libtomcrypt/src/headers/tomcrypt_private.h
lib/libtomcrypt/src/headers/tomcrypt_prng.h
lib/libtomcrypt/src/mac/blake2/blake2bmac.c
lib/libtomcrypt/src/mac/blake2/blake2bmac_file.c
lib/libtomcrypt/src/mac/blake2/blake2bmac_memory.c
lib/libtomcrypt/src/mac/blake2/blake2bmac_memory_multi.c
lib/libtomcrypt/src/mac/blake2/blake2bmac_test.c
lib/libtomcrypt/src/mac/blake2/blake2smac.c
lib/libtomcrypt/src/mac/blake2/blake2smac_file.c
lib/libtomcrypt/src/mac/blake2/blake2smac_memory.c
lib/libtomcrypt/src/mac/blake2/blake2smac_memory_multi.c
lib/libtomcrypt/src/mac/blake2/blake2smac_test.c
lib/libtomcrypt/src/mac/f9/f9_done.c
lib/libtomcrypt/src/mac/f9/f9_file.c
lib/libtomcrypt/src/mac/f9/f9_init.c
lib/libtomcrypt/src/mac/f9/f9_memory.c
lib/libtomcrypt/src/mac/f9/f9_memory_multi.c
lib/libtomcrypt/src/mac/f9/f9_process.c
lib/libtomcrypt/src/mac/f9/f9_test.c
lib/libtomcrypt/src/mac/hmac/hmac_done.c
lib/libtomcrypt/src/mac/hmac/hmac_file.c
lib/libtomcrypt/src/mac/hmac/hmac_init.c
lib/libtomcrypt/src/mac/hmac/hmac_memory.c
lib/libtomcrypt/src/mac/hmac/hmac_memory_multi.c
lib/libtomcrypt/src/mac/hmac/hmac_process.c
lib/libtomcrypt/src/mac/hmac/hmac_test.c
lib/libtomcrypt/src/mac/hmac/sub.mk
lib/libtomcrypt/src/mac/omac/omac_done.c
lib/libtomcrypt/src/mac/omac/omac_file.c
lib/libtomcrypt/src/mac/omac/omac_init.c
lib/libtomcrypt/src/mac/omac/omac_memory.c
lib/libtomcrypt/src/mac/omac/omac_memory_multi.c
lib/libtomcrypt/src/mac/omac/omac_process.c
lib/libtomcrypt/src/mac/omac/omac_test.c
lib/libtomcrypt/src/mac/omac/sub.mk
lib/libtomcrypt/src/mac/pelican/pelican.c
lib/libtomcrypt/src/mac/pelican/pelican_memory.c
lib/libtomcrypt/src/mac/pelican/pelican_test.c
lib/libtomcrypt/src/mac/pmac/pmac_done.c
lib/libtomcrypt/src/mac/pmac/pmac_file.c
lib/libtomcrypt/src/mac/pmac/pmac_init.c
lib/libtomcrypt/src/mac/pmac/pmac_memory.c
lib/libtomcrypt/src/mac/pmac/pmac_memory_multi.c
lib/libtomcrypt/src/mac/pmac/pmac_ntz.c
lib/libtomcrypt/src/mac/pmac/pmac_process.c
lib/libtomcrypt/src/mac/pmac/pmac_shift_xor.c
lib/libtomcrypt/src/mac/pmac/pmac_test.c
lib/libtomcrypt/src/mac/poly1305/poly1305.c
lib/libtomcrypt/src/mac/poly1305/poly1305_file.c
lib/libtomcrypt/src/mac/poly1305/poly1305_memory.c
lib/libtomcrypt/src/mac/poly1305/poly1305_memory_multi.c
lib/libtomcrypt/src/mac/poly1305/poly1305_test.c
lib/libtomcrypt/src/mac/xcbc/xcbc_done.c
lib/libtomcrypt/src/mac/xcbc/xcbc_file.c
lib/libtomcrypt/src/mac/xcbc/xcbc_init.c
lib/libtomcrypt/src/mac/xcbc/xcbc_memory.c
lib/libtomcrypt/src/mac/xcbc/xcbc_memory_multi.c
lib/libtomcrypt/src/mac/xcbc/xcbc_process.c
lib/libtomcrypt/src/mac/xcbc/xcbc_test.c
lib/libtomcrypt/src/math/fp/ltc_ecc_fp_mulmod.c
lib/libtomcrypt/src/math/gmp_desc.c
lib/libtomcrypt/src/math/ltm_desc.c
lib/libtomcrypt/src/math/multi.c
lib/libtomcrypt/src/math/radix_to_bin.c
lib/libtomcrypt/src/math/rand_bn.c
lib/libtomcrypt/src/math/rand_prime.c
lib/libtomcrypt/src/math/tfm_desc.c
lib/libtomcrypt/src/misc/adler32.c
lib/libtomcrypt/src/misc/base16/base16_decode.c
lib/libtomcrypt/src/misc/base16/base16_encode.c
lib/libtomcrypt/src/misc/base32/base32_decode.c
lib/libtomcrypt/src/misc/base32/base32_encode.c
lib/libtomcrypt/src/misc/base64/base64_decode.c
lib/libtomcrypt/src/misc/base64/base64_encode.c
lib/libtomcrypt/src/misc/burn_stack.c
lib/libtomcrypt/src/misc/compare_testvector.c
lib/libtomcrypt/src/misc/copy_or_zeromem.c
lib/libtomcrypt/src/misc/crc32.c
lib/libtomcrypt/src/misc/crypt/crypt.c
lib/libtomcrypt/src/misc/crypt/crypt_argchk.c
lib/libtomcrypt/src/misc/crypt/crypt_cipher_descriptor.c
lib/libtomcrypt/src/misc/crypt/crypt_cipher_is_valid.c
lib/libtomcrypt/src/misc/crypt/crypt_constants.c
lib/libtomcrypt/src/misc/crypt/crypt_find_cipher.c
lib/libtomcrypt/src/misc/crypt/crypt_find_cipher_any.c
lib/libtomcrypt/src/misc/crypt/crypt_find_cipher_id.c
lib/libtomcrypt/src/misc/crypt/crypt_find_hash.c
lib/libtomcrypt/src/misc/crypt/crypt_find_hash_any.c
lib/libtomcrypt/src/misc/crypt/crypt_find_hash_id.c
lib/libtomcrypt/src/misc/crypt/crypt_find_hash_oid.c
lib/libtomcrypt/src/misc/crypt/crypt_find_prng.c
lib/libtomcrypt/src/misc/crypt/crypt_fsa.c
lib/libtomcrypt/src/misc/crypt/crypt_hash_descriptor.c
lib/libtomcrypt/src/misc/crypt/crypt_hash_is_valid.c
lib/libtomcrypt/src/misc/crypt/crypt_inits.c
lib/libtomcrypt/src/misc/crypt/crypt_ltc_mp_descriptor.c
lib/libtomcrypt/src/misc/crypt/crypt_prng_descriptor.c
lib/libtomcrypt/src/misc/crypt/crypt_prng_is_valid.c
lib/libtomcrypt/src/misc/crypt/crypt_prng_rng_descriptor.c
lib/libtomcrypt/src/misc/crypt/crypt_register_all_ciphers.c
lib/libtomcrypt/src/misc/crypt/crypt_register_all_hashes.c
lib/libtomcrypt/src/misc/crypt/crypt_register_all_prngs.c
lib/libtomcrypt/src/misc/crypt/crypt_register_cipher.c
lib/libtomcrypt/src/misc/crypt/crypt_register_hash.c
lib/libtomcrypt/src/misc/crypt/crypt_register_prng.c
lib/libtomcrypt/src/misc/crypt/crypt_sizes.c
lib/libtomcrypt/src/misc/crypt/crypt_unregister_cipher.c
lib/libtomcrypt/src/misc/crypt/crypt_unregister_hash.c
lib/libtomcrypt/src/misc/crypt/crypt_unregister_prng.c
lib/libtomcrypt/src/misc/error_to_string.c
lib/libtomcrypt/src/misc/hkdf/hkdf.c
lib/libtomcrypt/src/misc/hkdf/hkdf_test.c
lib/libtomcrypt/src/misc/mem_neq.c
lib/libtomcrypt/src/misc/padding/padding_depad.c
lib/libtomcrypt/src/misc/padding/padding_pad.c
lib/libtomcrypt/src/misc/pbes/pbes.c
lib/libtomcrypt/src/misc/pbes/pbes1.c
lib/libtomcrypt/src/misc/pbes/pbes2.c
lib/libtomcrypt/src/misc/pkcs12/pkcs12_kdf.c
lib/libtomcrypt/src/misc/pkcs12/pkcs12_utf8_to_utf16.c
lib/libtomcrypt/src/misc/pkcs5/pkcs_5_1.c
lib/libtomcrypt/src/misc/pkcs5/pkcs_5_2.c
lib/libtomcrypt/src/misc/pkcs5/pkcs_5_test.c
lib/libtomcrypt/src/misc/ssh/ssh_decode_sequence_multi.c
lib/libtomcrypt/src/misc/ssh/ssh_encode_sequence_multi.c
lib/libtomcrypt/src/misc/ssh/sub.mk
lib/libtomcrypt/src/misc/sub.mk
lib/libtomcrypt/src/misc/zeromem.c
lib/libtomcrypt/src/modes/cbc/cbc_decrypt.c
lib/libtomcrypt/src/modes/cbc/cbc_done.c
lib/libtomcrypt/src/modes/cbc/cbc_encrypt.c
lib/libtomcrypt/src/modes/cbc/cbc_getiv.c
lib/libtomcrypt/src/modes/cbc/cbc_setiv.c
lib/libtomcrypt/src/modes/cbc/cbc_start.c
lib/libtomcrypt/src/modes/cfb/cfb_decrypt.c
lib/libtomcrypt/src/modes/cfb/cfb_done.c
lib/libtomcrypt/src/modes/cfb/cfb_encrypt.c
lib/libtomcrypt/src/modes/cfb/cfb_getiv.c
lib/libtomcrypt/src/modes/cfb/cfb_setiv.c
lib/libtomcrypt/src/modes/cfb/cfb_start.c
lib/libtomcrypt/src/modes/ctr/ctr_decrypt.c
lib/libtomcrypt/src/modes/ctr/ctr_done.c
lib/libtomcrypt/src/modes/ctr/ctr_encrypt.c
lib/libtomcrypt/src/modes/ctr/ctr_getiv.c
lib/libtomcrypt/src/modes/ctr/ctr_setiv.c
lib/libtomcrypt/src/modes/ctr/ctr_start.c
lib/libtomcrypt/src/modes/ctr/ctr_test.c
lib/libtomcrypt/src/modes/ctr/sub.mk
lib/libtomcrypt/src/modes/ecb/ecb_decrypt.c
lib/libtomcrypt/src/modes/ecb/ecb_done.c
lib/libtomcrypt/src/modes/ecb/ecb_encrypt.c
lib/libtomcrypt/src/modes/ecb/ecb_start.c
lib/libtomcrypt/src/modes/f8/f8_decrypt.c
lib/libtomcrypt/src/modes/f8/f8_done.c
lib/libtomcrypt/src/modes/f8/f8_encrypt.c
lib/libtomcrypt/src/modes/f8/f8_getiv.c
lib/libtomcrypt/src/modes/f8/f8_setiv.c
lib/libtomcrypt/src/modes/f8/f8_start.c
lib/libtomcrypt/src/modes/f8/f8_test_mode.c
lib/libtomcrypt/src/modes/lrw/lrw_decrypt.c
lib/libtomcrypt/src/modes/lrw/lrw_done.c
lib/libtomcrypt/src/modes/lrw/lrw_encrypt.c
lib/libtomcrypt/src/modes/lrw/lrw_getiv.c
lib/libtomcrypt/src/modes/lrw/lrw_process.c
lib/libtomcrypt/src/modes/lrw/lrw_setiv.c
lib/libtomcrypt/src/modes/lrw/lrw_start.c
lib/libtomcrypt/src/modes/lrw/lrw_test.c
lib/libtomcrypt/src/modes/lrw/sub.mk
lib/libtomcrypt/src/modes/ofb/ofb_decrypt.c
lib/libtomcrypt/src/modes/ofb/ofb_done.c
lib/libtomcrypt/src/modes/ofb/ofb_encrypt.c
lib/libtomcrypt/src/modes/ofb/ofb_getiv.c
lib/libtomcrypt/src/modes/ofb/ofb_setiv.c
lib/libtomcrypt/src/modes/ofb/ofb_start.c
lib/libtomcrypt/src/modes/xts/sub.mk
lib/libtomcrypt/src/modes/xts/xts_decrypt.c
lib/libtomcrypt/src/modes/xts/xts_done.c
lib/libtomcrypt/src/modes/xts/xts_encrypt.c
lib/libtomcrypt/src/modes/xts/xts_init.c
lib/libtomcrypt/src/modes/xts/xts_mult_x.c
lib/libtomcrypt/src/modes/xts/xts_test.c
lib/libtomcrypt/src/pk/asn1/der/bit/der_decode_bit_string.c
lib/libtomcrypt/src/pk/asn1/der/bit/der_decode_raw_bit_string.c
lib/libtomcrypt/src/pk/asn1/der/bit/der_encode_bit_string.c
lib/libtomcrypt/src/pk/asn1/der/bit/der_encode_raw_bit_string.c
lib/libtomcrypt/src/pk/asn1/der/bit/der_length_bit_string.c
lib/libtomcrypt/src/pk/asn1/der/boolean/der_decode_boolean.c
lib/libtomcrypt/src/pk/asn1/der/boolean/der_encode_boolean.c
lib/libtomcrypt/src/pk/asn1/der/boolean/der_length_boolean.c
lib/libtomcrypt/src/pk/asn1/der/choice/der_decode_choice.c
lib/libtomcrypt/src/pk/asn1/der/custom_type/der_decode_custom_type.c
lib/libtomcrypt/src/pk/asn1/der/custom_type/der_encode_custom_type.c
lib/libtomcrypt/src/pk/asn1/der/custom_type/der_length_custom_type.c
lib/libtomcrypt/src/pk/asn1/der/custom_type/sub.mk
lib/libtomcrypt/src/pk/asn1/der/general/der_asn1_maps.c
lib/libtomcrypt/src/pk/asn1/der/general/der_decode_asn1_identifier.c
lib/libtomcrypt/src/pk/asn1/der/general/der_decode_asn1_length.c
lib/libtomcrypt/src/pk/asn1/der/general/der_encode_asn1_identifier.c
lib/libtomcrypt/src/pk/asn1/der/general/der_encode_asn1_length.c
lib/libtomcrypt/src/pk/asn1/der/general/der_length_asn1_identifier.c
lib/libtomcrypt/src/pk/asn1/der/general/der_length_asn1_length.c
lib/libtomcrypt/src/pk/asn1/der/general/sub.mk
lib/libtomcrypt/src/pk/asn1/der/generalizedtime/der_decode_generalizedtime.c
lib/libtomcrypt/src/pk/asn1/der/generalizedtime/der_encode_generalizedtime.c
lib/libtomcrypt/src/pk/asn1/der/generalizedtime/der_length_generalizedtime.c
lib/libtomcrypt/src/pk/asn1/der/generalizedtime/sub.mk
lib/libtomcrypt/src/pk/asn1/der/ia5/der_decode_ia5_string.c
lib/libtomcrypt/src/pk/asn1/der/ia5/der_encode_ia5_string.c
lib/libtomcrypt/src/pk/asn1/der/ia5/der_length_ia5_string.c
lib/libtomcrypt/src/pk/asn1/der/integer/der_decode_integer.c
lib/libtomcrypt/src/pk/asn1/der/integer/der_encode_integer.c
lib/libtomcrypt/src/pk/asn1/der/integer/der_length_integer.c
lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_decode_object_identifier.c
lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_encode_object_identifier.c
lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_length_object_identifier.c
lib/libtomcrypt/src/pk/asn1/der/octet/der_decode_octet_string.c
lib/libtomcrypt/src/pk/asn1/der/octet/der_encode_octet_string.c
lib/libtomcrypt/src/pk/asn1/der/octet/der_length_octet_string.c
lib/libtomcrypt/src/pk/asn1/der/printable_string/der_decode_printable_string.c
lib/libtomcrypt/src/pk/asn1/der/printable_string/der_encode_printable_string.c
lib/libtomcrypt/src/pk/asn1/der/printable_string/der_length_printable_string.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_ex.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_flexi.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_multi.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_encode_sequence_ex.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_encode_sequence_multi.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_length_sequence.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_sequence_free.c
lib/libtomcrypt/src/pk/asn1/der/sequence/der_sequence_shrink.c
lib/libtomcrypt/src/pk/asn1/der/sequence/sub.mk
lib/libtomcrypt/src/pk/asn1/der/set/der_encode_set.c
lib/libtomcrypt/src/pk/asn1/der/set/der_encode_setof.c
lib/libtomcrypt/src/pk/asn1/der/short_integer/der_decode_short_integer.c
lib/libtomcrypt/src/pk/asn1/der/short_integer/der_encode_short_integer.c
lib/libtomcrypt/src/pk/asn1/der/short_integer/der_length_short_integer.c
lib/libtomcrypt/src/pk/asn1/der/sub.mk
lib/libtomcrypt/src/pk/asn1/der/teletex_string/der_decode_teletex_string.c
lib/libtomcrypt/src/pk/asn1/der/teletex_string/der_length_teletex_string.c
lib/libtomcrypt/src/pk/asn1/der/utctime/der_decode_utctime.c
lib/libtomcrypt/src/pk/asn1/der/utctime/der_encode_utctime.c
lib/libtomcrypt/src/pk/asn1/der/utctime/der_length_utctime.c
lib/libtomcrypt/src/pk/asn1/der/utf8/der_decode_utf8_string.c
lib/libtomcrypt/src/pk/asn1/der/utf8/der_encode_utf8_string.c
lib/libtomcrypt/src/pk/asn1/der/utf8/der_length_utf8_string.c
lib/libtomcrypt/src/pk/asn1/oid/pk_get_oid.c
lib/libtomcrypt/src/pk/asn1/oid/pk_oid_cmp.c
lib/libtomcrypt/src/pk/asn1/oid/pk_oid_str.c
lib/libtomcrypt/src/pk/asn1/oid/sub.mk
lib/libtomcrypt/src/pk/asn1/pkcs8/pkcs8_decode_flexi.c
lib/libtomcrypt/src/pk/asn1/sub.mk
lib/libtomcrypt/src/pk/asn1/x509/x509_decode_public_key_from_certificate.c
lib/libtomcrypt/src/pk/asn1/x509/x509_decode_subject_public_key_info.c
lib/libtomcrypt/src/pk/asn1/x509/x509_encode_subject_public_key_info.c
lib/libtomcrypt/src/pk/dh/dh.c
lib/libtomcrypt/src/pk/dh/dh_check_pubkey.c
lib/libtomcrypt/src/pk/dh/dh_export.c
lib/libtomcrypt/src/pk/dh/dh_export_key.c
lib/libtomcrypt/src/pk/dh/dh_free.c
lib/libtomcrypt/src/pk/dh/dh_generate_key.c
lib/libtomcrypt/src/pk/dh/dh_import.c
lib/libtomcrypt/src/pk/dh/dh_make_key.c
lib/libtomcrypt/src/pk/dh/dh_set.c
lib/libtomcrypt/src/pk/dh/dh_set_pg_dhparam.c
lib/libtomcrypt/src/pk/dh/dh_shared_secret.c
lib/libtomcrypt/src/pk/dh/sub.mk
lib/libtomcrypt/src/pk/dsa/dsa_decrypt_key.c
lib/libtomcrypt/src/pk/dsa/dsa_encrypt_key.c
lib/libtomcrypt/src/pk/dsa/dsa_export.c
lib/libtomcrypt/src/pk/dsa/dsa_free.c
lib/libtomcrypt/src/pk/dsa/dsa_generate_key.c
lib/libtomcrypt/src/pk/dsa/dsa_generate_pqg.c
lib/libtomcrypt/src/pk/dsa/dsa_import.c
lib/libtomcrypt/src/pk/dsa/dsa_make_key.c
lib/libtomcrypt/src/pk/dsa/dsa_set.c
lib/libtomcrypt/src/pk/dsa/dsa_set_pqg_dsaparam.c
lib/libtomcrypt/src/pk/dsa/dsa_shared_secret.c
lib/libtomcrypt/src/pk/dsa/dsa_sign_hash.c
lib/libtomcrypt/src/pk/dsa/dsa_verify_hash.c
lib/libtomcrypt/src/pk/dsa/dsa_verify_key.c
lib/libtomcrypt/src/pk/dsa/sub.mk
lib/libtomcrypt/src/pk/ec25519/ec25519_export.c
lib/libtomcrypt/src/pk/ec25519/ec25519_import_pkcs8.c
lib/libtomcrypt/src/pk/ec25519/tweetnacl.c
lib/libtomcrypt/src/pk/ecc/ecc.c
lib/libtomcrypt/src/pk/ecc/ecc_ansi_x963_export.c
lib/libtomcrypt/src/pk/ecc/ecc_ansi_x963_import.c
lib/libtomcrypt/src/pk/ecc/ecc_decrypt_key.c
lib/libtomcrypt/src/pk/ecc/ecc_encrypt_key.c
lib/libtomcrypt/src/pk/ecc/ecc_export.c
lib/libtomcrypt/src/pk/ecc/ecc_export_openssl.c
lib/libtomcrypt/src/pk/ecc/ecc_find_curve.c
lib/libtomcrypt/src/pk/ecc/ecc_free.c
lib/libtomcrypt/src/pk/ecc/ecc_get_key.c
lib/libtomcrypt/src/pk/ecc/ecc_get_oid_str.c
lib/libtomcrypt/src/pk/ecc/ecc_get_size.c
lib/libtomcrypt/src/pk/ecc/ecc_import.c
lib/libtomcrypt/src/pk/ecc/ecc_import_openssl.c
lib/libtomcrypt/src/pk/ecc/ecc_import_pkcs8.c
lib/libtomcrypt/src/pk/ecc/ecc_import_x509.c
lib/libtomcrypt/src/pk/ecc/ecc_make_key.c
lib/libtomcrypt/src/pk/ecc/ecc_recover_key.c
lib/libtomcrypt/src/pk/ecc/ecc_set_curve.c
lib/libtomcrypt/src/pk/ecc/ecc_set_curve_internal.c
lib/libtomcrypt/src/pk/ecc/ecc_set_key.c
lib/libtomcrypt/src/pk/ecc/ecc_shared_secret.c
lib/libtomcrypt/src/pk/ecc/ecc_sign_hash.c
lib/libtomcrypt/src/pk/ecc/ecc_sizes.c
lib/libtomcrypt/src/pk/ecc/ecc_ssh_ecdsa_encode_name.c
lib/libtomcrypt/src/pk/ecc/ecc_verify_hash.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_export_point.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_import_point.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_is_point.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_is_point_at_infinity.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_map.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_mul2add.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_mulmod.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_mulmod_timing.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_points.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_projective_add_point.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_projective_dbl_point.c
lib/libtomcrypt/src/pk/ecc/ltc_ecc_verify_key.c
lib/libtomcrypt/src/pk/ecc/sub.mk
lib/libtomcrypt/src/pk/ed25519/ed25519_export.c
lib/libtomcrypt/src/pk/ed25519/ed25519_import.c
lib/libtomcrypt/src/pk/ed25519/ed25519_import_pkcs8.c
lib/libtomcrypt/src/pk/ed25519/ed25519_import_x509.c
lib/libtomcrypt/src/pk/ed25519/ed25519_make_key.c
lib/libtomcrypt/src/pk/ed25519/ed25519_set_key.c
lib/libtomcrypt/src/pk/ed25519/ed25519_sign.c
lib/libtomcrypt/src/pk/ed25519/ed25519_verify.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_i2osp.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_mgf1.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_oaep_decode.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_oaep_encode.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_os2ip.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_pss_decode.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_pss_encode.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_v1_5_decode.c
lib/libtomcrypt/src/pk/pkcs1/pkcs_1_v1_5_encode.c
lib/libtomcrypt/src/pk/rsa/rsa_decrypt_key.c
lib/libtomcrypt/src/pk/rsa/rsa_encrypt_key.c
lib/libtomcrypt/src/pk/rsa/rsa_export.c
lib/libtomcrypt/src/pk/rsa/rsa_exptmod.c
lib/libtomcrypt/src/pk/rsa/rsa_free.c
lib/libtomcrypt/src/pk/rsa/rsa_get_size.c
lib/libtomcrypt/src/pk/rsa/rsa_import.c
lib/libtomcrypt/src/pk/rsa/rsa_import_pkcs8.c
lib/libtomcrypt/src/pk/rsa/rsa_import_x509.c
lib/libtomcrypt/src/pk/rsa/rsa_make_key.c
lib/libtomcrypt/src/pk/rsa/rsa_set.c
lib/libtomcrypt/src/pk/rsa/rsa_sign_hash.c
lib/libtomcrypt/src/pk/rsa/rsa_sign_saltlen_get.c
lib/libtomcrypt/src/pk/rsa/rsa_verify_hash.c
lib/libtomcrypt/src/pk/x25519/x25519_export.c
lib/libtomcrypt/src/pk/x25519/x25519_import.c
lib/libtomcrypt/src/pk/x25519/x25519_import_pkcs8.c
lib/libtomcrypt/src/pk/x25519/x25519_import_x509.c
lib/libtomcrypt/src/pk/x25519/x25519_make_key.c
lib/libtomcrypt/src/pk/x25519/x25519_set_key.c
lib/libtomcrypt/src/pk/x25519/x25519_shared_secret.c
lib/libtomcrypt/src/prngs/chacha20.c
lib/libtomcrypt/src/prngs/fortuna.c
lib/libtomcrypt/src/prngs/rc4.c
lib/libtomcrypt/src/prngs/rng_get_bytes.c
lib/libtomcrypt/src/prngs/rng_make_prng.c
lib/libtomcrypt/src/prngs/sober128.c
lib/libtomcrypt/src/prngs/sprng.c
lib/libtomcrypt/src/prngs/yarrow.c
lib/libtomcrypt/src/stream/chacha/chacha_crypt.c
lib/libtomcrypt/src/stream/chacha/chacha_done.c
lib/libtomcrypt/src/stream/chacha/chacha_ivctr32.c
lib/libtomcrypt/src/stream/chacha/chacha_ivctr64.c
lib/libtomcrypt/src/stream/chacha/chacha_keystream.c
lib/libtomcrypt/src/stream/chacha/chacha_memory.c
lib/libtomcrypt/src/stream/chacha/chacha_setup.c
lib/libtomcrypt/src/stream/chacha/chacha_test.c
lib/libtomcrypt/src/stream/rabbit/rabbit.c
lib/libtomcrypt/src/stream/rabbit/rabbit_memory.c
lib/libtomcrypt/src/stream/rc4/rc4_stream.c
lib/libtomcrypt/src/stream/rc4/rc4_stream_memory.c
lib/libtomcrypt/src/stream/rc4/rc4_test.c
lib/libtomcrypt/src/stream/salsa20/salsa20_crypt.c
lib/libtomcrypt/src/stream/salsa20/salsa20_done.c
lib/libtomcrypt/src/stream/salsa20/salsa20_ivctr64.c
lib/libtomcrypt/src/stream/salsa20/salsa20_keystream.c
lib/libtomcrypt/src/stream/salsa20/salsa20_memory.c
lib/libtomcrypt/src/stream/salsa20/salsa20_setup.c
lib/libtomcrypt/src/stream/salsa20/salsa20_test.c
lib/libtomcrypt/src/stream/salsa20/xsalsa20_memory.c
lib/libtomcrypt/src/stream/salsa20/xsalsa20_setup.c
lib/libtomcrypt/src/stream/salsa20/xsalsa20_test.c
lib/libtomcrypt/src/stream/sober128/sober128_stream.c
lib/libtomcrypt/src/stream/sober128/sober128_stream_memory.c
lib/libtomcrypt/src/stream/sober128/sober128_test.c
lib/libtomcrypt/src/stream/sober128/sober128tab.c
lib/libtomcrypt/src/stream/sosemanuk/sosemanuk.c
lib/libtomcrypt/src/stream/sosemanuk/sosemanuk_memory.c
lib/libtomcrypt/src/stream/sosemanuk/sosemanuk_test.c
lib/libtomcrypt/sub.mk
lib/libtomcrypt/tomcrypt.c
lib/libtomcrypt/xts.c
/optee_os/ldelf/ta_elf_rel.c
/optee_os/lib/libutils/ext/include/compiler.h
27e1949910-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: ltc: force alignment of A32 assembler functions to 4 bytes

The Clang assembler will not align all the functions containing A32
code (as opposed to thumb) on 4-byte boundaries, contrary to GCC.

core: ltc: force alignment of A32 assembler functions to 4 bytes

The Clang assembler will not align all the functions containing A32
code (as opposed to thumb) on 4-byte boundaries, contrary to GCC.
This can cause a runtime exception (undef-abort).

Add a ".balign 4" to the ENTRY macro to fix that.

See also commit ff7c2da6d14b ("Force alignment of assembler functions
(FUNC and LOCAL_FUNC) to 4 bytes") [1].

Link: [1] https://github.com/OP-TEE/optee_os/commit/ff7c2da6d14b
Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

bb1d5c3210-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: ltc: aes_modes_armv8a_ce_a64.S: get rid of literal load of addend vector

Cherry pick of Linux kernel commit ed6ed11830a9 ("crypto:
arm64/aes-modes - get rid of literal load of addend vector").

core: ltc: aes_modes_armv8a_ce_a64.S: get rid of literal load of addend vector

Cherry pick of Linux kernel commit ed6ed11830a9 ("crypto:
arm64/aes-modes - get rid of literal load of addend vector"). Original
commit message:

"
Replace the literal load of the addend vector with a sequence that
performs each add individually. This sequence is only 2 instructions
longer than the original, and 2% faster on Cortex-A53.

This is an improvement by itself, but also works around a Clang issue,
whose integrated assembler does not implement the GNU ARM asm syntax
completely, and does not support the =literal notation for FP registers
(more info at https://bugs.llvm.org/show_bug.cgi?id=38642)
"

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>
Acked-by: Ard Biesheuvel <ard.biesheuvel@linaro.org>

show more ...

f749239110-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: ltc: aes_modes_armv8a_ce_a64.S: fix incorrect assembly syntax

"umov w0, v0.4s[0]" is not valid UAL syntax; the 4 should not be here.
GCC accepts it fine but Clang does not. Fix it.

Signed-off

core: ltc: aes_modes_armv8a_ce_a64.S: fix incorrect assembly syntax

"umov w0, v0.4s[0]" is not valid UAL syntax; the 4 should not be here.
GCC accepts it fine but Clang does not. Fix it.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

69e57dcf10-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: arm64: crypto: AES-GCM: fix incorrect assembly syntax

"umov w0, v0.4s[0]" is not valid UAL syntax; the 4 should not be here.
GCC accepts it fine but Clang does not. Fix it.

Signed-off-by: Jer

core: arm64: crypto: AES-GCM: fix incorrect assembly syntax

"umov w0, v0.4s[0]" is not valid UAL syntax; the 4 should not be here.
GCC accepts it fine but Clang does not. Fix it.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

1e86658810-Sep-2019 Jerome Forissier <jerome@forissier.org>

core: dt: add __noreturn to _fdt_fill_device_info() stub

When CFG_DT != y, the stub function _fdt_fill_device_info() just
panics. Therefore it deserves the __noreturn attribute. Adding it makes
a Cl

core: dt: add __noreturn to _fdt_fill_device_info() stub

When CFG_DT != y, the stub function _fdt_fill_device_info() just
panics. Therefore it deserves the __noreturn attribute. Adding it makes
a Clang warning go away.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

f8f95bc110-Sep-2019 Jerome Forissier <jerome@forissier.org>

Get rid of option -Wno-suggest-attribute=noreturn

The GCC option -Wno-suggest-attribute=noreturn is not supported by
Clang. Instead of playing with compiler options, let's fix the code
according to

Get rid of option -Wno-suggest-attribute=noreturn

The GCC option -Wno-suggest-attribute=noreturn is not supported by
Clang. Instead of playing with compiler options, let's fix the code
according to the following rules:
- If a function is know to never return, it should have the __noreturn
attribute in the header file.
- If only some implementation of a function never returns, __noreturn
shall be applied to that particular implementation in the .c file.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

7222fc6a06-Aug-2019 Cedric Neveux <cedric.neveux@nxp.com>

core: driver: generic resources for crypto device driver

Add a generic cryptographic driver interface connecting
TEE Crypto generic APIs to HW driver interface

The Generic Crypto Driver interface i

core: driver: generic resources for crypto device driver

Add a generic cryptographic driver interface connecting
TEE Crypto generic APIs to HW driver interface

The Generic Crypto Driver interface in the core/driver/crypto/crypto_api
is implemented to be able to use a HW driver.

Signed-off-by: Cedric Neveux <cedric.neveux@nxp.com>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Jerome Forissier <jerome@forissier.org>

show more ...

1df107b603-Sep-2019 Sumit Garg <sumit.garg@linaro.org>

ftrace: exclude only foreign interrupt time

Current TA function execution time feature only reports user mode
execution time and exclude any non-user mode execution time. But in
case of syscalls whi

ftrace: exclude only foreign interrupt time

Current TA function execution time feature only reports user mode
execution time and exclude any non-user mode execution time. But in
case of syscalls which are essentially function invocations from TA
into the kernel, we shouldn't exclude syscall execution time in order
to account for actual function execution time. That means we only
exclude time that is spent serving foreign interrupts.

So changes in this patch allows to incorporate syscall execution time
in the function graph output.

Fixes: f5df167c2ffb ("ftrace: Add function execution time support")
Signed-off-by: Sumit Garg <sumit.garg@linaro.org>
Acked-by: Jerome Forissier <jerome@forissier.org>

show more ...

a28e3d9d04-Sep-2019 Jerome Forissier <jerome@forissier.org>

hikey960: add ASAN shadow offset for 32-bit build

Adds the proper CFG_ASAN_SHADOW_OFFSET value for HiKey960 in 32-bit
mode. This allows to run with the kernel address sanitizer enabled
(CFG_CORE_SAN

hikey960: add ASAN shadow offset for 32-bit build

Adds the proper CFG_ASAN_SHADOW_OFFSET value for HiKey960 in 32-bit
mode. This allows to run with the kernel address sanitizer enabled
(CFG_CORE_SANITIZE_KADDRESS=y).

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

f5ae8b2928-Aug-2019 Ricardo Salveti <ricardo@foundries.io>

core: imx: add mx6dapalis/mx6qapalis platform flavor

Add Toradex Apalis iMX6D and iMX6Q (1GB module variant) platform
flavors.

CFG_DDR_SIZE needs to be manually set by the user (e.g. 0x80000000)
if

core: imx: add mx6dapalis/mx6qapalis platform flavor

Add Toradex Apalis iMX6D and iMX6Q (1GB module variant) platform
flavors.

CFG_DDR_SIZE needs to be manually set by the user (e.g. 0x80000000)
if using the 2GB module variants.

Signed-off-by: Ricardo Salveti <ricardo@foundries.io>
Reviewed-by: Rouven Czerwinski <r.czerwinski@pengutronix.de>
Acked-by: Jerome Forissier <jerome@forissier.org>

show more ...

f795b67312-Aug-2019 Clement Faure <clement.faure@nxp.com>

core: imx: add support for i.MX 8MN

Add support for i.MX 8MN.
Add board flavor:
* imx8mnevk

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@lin

core: imx: add support for i.MX 8MN

Add support for i.MX 8MN.
Add board flavor:
* imx8mnevk

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

bacb1a4b22-Nov-2018 Silvano di Ninno <silvano.dininno@nxp.com>

core: imx: add support for i.MX 8QM

Add support for i.MX 8QM.
Add board flavors:
* imx8qmmek

Signed-off-by: Silvano di Ninno <silvano.dininno@nxp.com>
Signed-off-by: Clement Faure <clement.faure@n

core: imx: add support for i.MX 8QM

Add support for i.MX 8QM.
Add board flavors:
* imx8qmmek

Signed-off-by: Silvano di Ninno <silvano.dininno@nxp.com>
Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

d3bf580a22-Nov-2018 Silvano di Ninno <silvano.dininno@nxp.com>

core: imx: add support for i.MX 8QxP

Add support for i.MX 8QxP
Add board flavors:
* imx8qxpmek

Signed-off-by: Silvano di Ninno <silvano.dininno@nxp.com>
Signed-off-by: Alessandro Di Chiara <alessa

core: imx: add support for i.MX 8QxP

Add support for i.MX 8QxP
Add board flavors:
* imx8qxpmek

Signed-off-by: Silvano di Ninno <silvano.dininno@nxp.com>
Signed-off-by: Alessandro Di Chiara <alessandro.dichiara@nxp.com>
Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

ada502b812-Aug-2019 Clement Faure <clement.faure@nxp.com>

core: imx: allow to boot without console

Allow imx SoCs to boot without console when CONSOLE_UART_BASE is not
defined.

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Foris

core: imx: allow to boot without console

Allow imx SoCs to boot without console when CONSOLE_UART_BASE is not
defined.

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

f1c2959f12-Aug-2019 Clement Faure <clement.faure@nxp.com>

core: imx: add device tree support for uart

Allow driver to read device tree to enable uart.

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@lin

core: imx: add device tree support for uart

Allow driver to read device tree to enable uart.

Signed-off-by: Clement Faure <clement.faure@nxp.com>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

2f6dffbd02-Sep-2019 Jerome Forissier <jerome@forissier.org>

build: do not use -Wp with the preprocessor and use -o instead of a redirection

This patch cleans up the command line where we use the C preprocessor
to better reflect the documented usage in the GC

build: do not use -Wp with the preprocessor and use -o instead of a redirection

This patch cleans up the command line where we use the C preprocessor
to better reflect the documented usage in the GCC man page, thus
preparing for Clang support.

1. When invoking the C preprocessor, there is no need for -Wp to pass
arguments, so remove it.

2. -MD is not supposed to take a file name when passed to cpp. The
dependency output file name is overridden with -MF.

3. Lastly, it is better to use -o to specify the output file instead
of redirecting standard output, because if an error occurs during
preprocessing we don't want the output file to be created.

Signed-off-by: Jerome Forissier <jerome@forissier.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

b516aa9729-Aug-2019 Rouven Czerwinski <r.czerwinski@pengutronix.de>

core: add missing arch_extension to thread assembly

Compilation with newer gcc versions fails:

core/arch/arm/kernel/thread_optee_smc_a32.S: Assembler messages:
core/arch/arm/kernel/thread_optee_smc

core: add missing arch_extension to thread assembly

Compilation with newer gcc versions fails:

core/arch/arm/kernel/thread_optee_smc_a32.S: Assembler messages:
core/arch/arm/kernel/thread_optee_smc_a32.S:29: Error: selected processor does not support `smc #0' in ARM mode

add the required .arch_extension sec to the recently added assembly
file.

Fixes: 2786f1438fc8 ("core: thread: separate old SMC interface handling")
Signed-off-by: Rouven Czerwinski <r.czerwinski@pengutronix.de>
Reviewed-by: Jerome Forissier <jerome@forissier.org>

show more ...

776d215826-Jun-2019 Rouven Czerwinski <r.czerwinski@pengutronix.de>

core: import IS_ENABLED macro from Zephyr OS

The IS_ENABLED macro checks whether a macro is defined to the value
1 or may not be defined at all. This allows checks in the code instead
of using #ifde

core: import IS_ENABLED macro from Zephyr OS

The IS_ENABLED macro checks whether a macro is defined to the value
1 or may not be defined at all. This allows checks in the code instead
of using #ifdef:

#define CFG_MX6Q 1

if (IS_ENABLED(CFG_MX6Q))
printf("MX6Q enabled")
if (IS_ENABLED(CFG_MX6D))
printf("MX6D enabled")

expands to:

if (1)
printf("MX6Q enabled")
if (0)
printf("MX6Q enabled")

where the second if statement can be optimized out by the compiler.

This implementation was imported from Zephyr OS commit
ff07fc7f0a19 ("lib: libc: fix alignment of HEAP base address for ARM").

The Copyright is attributed to Intel, since the original
commit 5bc458a0fae5 ("util.h: Add IS_ENABLED() macro for
expression-legal ifdef-checking") was done by Andy Ross
<andrew.j.ross@intel.com>.

Signed-off-by: Rouven Czerwinski <r.czerwinski@pengutronix.de>
Acked-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>
Reviewed-by: Peng Fan <peng.fan@nxp.com>

show more ...

c462c67402-Aug-2019 Cedric Neveux <cedric.neveux@nxp.com>

core: arm64: add read_ctr_el0 function

Add the read_ctr_el0 function in the arm64.h file

Signed-off-by: Cedric Neveux <cedric.neveux@nxp.com>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

1...<<161162163164165166167168169170>>...259