History log of /optee_os/core/arch/ (Results 2926 – 2950 of 4033)
Revision Date Author Comments
(<<< Hide modified files)
(Show modified files >>>)
27c1d9a712-Jan-2018 Jerome Forissier <jerome.forissier@linaro.org>

core: lpae: mask exceptions during core_mmu_find_table()

core_mmu_find_table() calls get_core_pos() so it should mask interrupts
to avoid being re-scheduled to another core.

Signed-off-by: Jerome F

core: lpae: mask exceptions during core_mmu_find_table()

core_mmu_find_table() calls get_core_pos() so it should mask interrupts
to avoid being re-scheduled to another core.

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

show more ...

5ff5a48e12-Jan-2018 Jens Wiklander <jens.wiklander@linaro.org>

core: thread: fix exception return

Fixes exception return from FIQ and SVC handlers to not return via
abort mode as we under some circumstances may return to abort mode.

Fixes: 5b8a58b415da ("core:

core: thread: fix exception return

Fixes exception return from FIQ and SVC handlers to not return via
abort mode as we under some circumstances may return to abort mode.

Fixes: 5b8a58b415da ("core: thread: fix exception return")
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

6e093e3115-Jan-2018 Jens Wiklander <jens.wiklander@linaro.org>

core: thread_a64.S: fix gcc 4.9 compile error

Fixes compile errors
out/arm-plat-hikey/core/arch/arm/kernel/thread_a64.o: In function `el0_sync_abort':
/home/bla/optee_os/core/arch/arm/kernel/thread_

core: thread_a64.S: fix gcc 4.9 compile error

Fixes compile errors
out/arm-plat-hikey/core/arch/arm/kernel/thread_a64.o: In function `el0_sync_abort':
/home/bla/optee_os/core/arch/arm/kernel/thread_a64.S:778:(.text.el0_sync_abort+0xf4): relocation truncated to fit: R_AARCH64_TSTBR14 against `.text.thread_vect_table'
out/arm-plat-hikey/core/arch/arm/kernel/thread_a64.o: In function `elx_fiq':
/home/bla/optee_os/core/arch/arm/kernel/thread_a64.S:949:(.text.elx_fiq+0x9c): relocation truncated to fit: R_AARCH64_TSTBR14 against `.text.thread_vect_table'
make: *** [out/arm-plat-hikey/core/tee.elf] Error 1
experienced with some gcc 4.9 compiler

Fixes: https://github.com/OP-TEE/optee_os/issues/2067
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Tested-by: Victor Chong <victor.chong@linaro.org> (hikey)
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

a235648612-Jan-2018 Peng Fan <peng.fan@nxp.com>

arm: pl310: fix cache sync

According to PL310 TRM:
Atomic operations:
The following are atomic operations:
Clean Line by PA or by Set/Way
Invalidate Line by PA
Clean and Invalidate Line

arm: pl310: fix cache sync

According to PL310 TRM:
Atomic operations:
The following are atomic operations:
Clean Line by PA or by Set/Way
Invalidate Line by PA
Clean and Invalidate Line by PA or by Set/Way
Cache Sync.
These operations stall the slave ports until they are complete.
When these registers are read, bit [0], the C flag, indicates that
a background operation is in progress. When written, bit 0 must be
zero.

So write 1 to sync register is not correct.

Signed-off-by: Peng Fan <peng.fan@nxp.com>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>

show more ...

8f643c0011-Jan-2018 Jerome Forissier <jerome.forissier@linaro.org>

core: crypto: default enable HWSUPP_PMULT_64 with CRYPTO_WITH_CE

64-bit polynomial multiply is defined in the ARMv8.0 Cryptographic
Extension instructions together with other instructions like AES*

core: crypto: default enable HWSUPP_PMULT_64 with CRYPTO_WITH_CE

64-bit polynomial multiply is defined in the ARMv8.0 Cryptographic
Extension instructions together with other instructions like AES*
and SHA1*. Therefore, it is reasonable to enable CFG_HWSUPP_PMULT_64
when CFG_CRYPTO_WITH_CE is enabled. Platforms can always override this
value if need be.

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

show more ...

6d0fd33111-Jan-2018 Jerome Forissier <jerome.forissier@linaro.org>

core: crypto: rename CFG_HWSUPP_PMULL to CFG_HWSUPP_PMULT_64

CFG_HWSUPP_PMULL is used to determine whether the CPU supports long
polynomial multiplies of 64-bit values, which means:
- for AArch64: P

core: crypto: rename CFG_HWSUPP_PMULL to CFG_HWSUPP_PMULT_64

CFG_HWSUPP_PMULL is used to determine whether the CPU supports long
polynomial multiplies of 64-bit values, which means:
- for AArch64: PMULL and PMULL2 with the 1Q arrangement specifier
- for AArch32: VMULL.P64
Otherwise, 8-bit polynomial multiplication is used instead.

Therefore, CFG_HWSUPP_PMULT_64 is a better name because it does not
seem to imply Aarch64 (no PMULL) and clearly states the 64-bit size.

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

show more ...

ecf2e01421-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: crypto.h manages hash context memory

To ease integration with other crypto libraries change the hash context
interface in crypto.h to manage the memory used for the hash context.

Reviewed-by:

core: crypto.h manages hash context memory

To ease integration with other crypto libraries change the hash context
interface in crypto.h to manage the memory used for the hash context.

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

show more ...

b1d7375c15-Dec-2017 Jerome Forissier <jerome.forissier@linaro.org>

Remove 'All rights reserved' from Linaro files

The text 'All rights reserved' is useless [1]. The Free Software
Foundation's REUSE Initiative best practices document [2] does not
contain these words

Remove 'All rights reserved' from Linaro files

The text 'All rights reserved' is useless [1]. The Free Software
Foundation's REUSE Initiative best practices document [2] does not
contain these words. Therefore, we can safely remove the text from the
files that are owned by Linaro.

Generated by:
spdxify.py --linaro-only --strip-arr optee_os/

Link: [1] https://en.wikipedia.org/wiki/All_rights_reserved
Link: [2] https://reuse.software/practices/
Link: [3] https://github.com/jforissier/misc/blob/f7b56c8/spdxify.py
Signed-off-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Joakim Bech <joakim.bech@linaro.org>

show more ...


arm/include/arm.h
arm/include/arm64.h
arm/include/arm64_macros.S
arm/include/kernel/abort.h
arm/include/kernel/cache_helpers.h
arm/include/kernel/early_ta.h
arm/include/kernel/generic_boot.h
arm/include/kernel/linker.h
arm/include/kernel/mutex.h
arm/include/kernel/pm_stubs.h
arm/include/kernel/pseudo_ta.h
arm/include/kernel/time_source.h
arm/include/kernel/user_ta.h
arm/include/kernel/vfp.h
arm/include/kernel/wait_queue.h
arm/include/mm/mobj.h
arm/include/mm/pgt_cache.h
arm/include/sm/optee_smc.h
arm/include/sm/teesmc_opteed.h
arm/include/sm/teesmc_opteed_macros.h
arm/include/tee/arch_svc.h
arm/kernel/abort.c
arm/kernel/asm-defines.c
arm/kernel/early_ta.c
arm/kernel/elf_load.c
arm/kernel/elf_load.h
arm/kernel/generic_boot.c
arm/kernel/generic_entry_a32.S
arm/kernel/generic_entry_a64.S
arm/kernel/link_dummies.c
arm/kernel/link_dummy.ld
arm/kernel/misc_a64.S
arm/kernel/mutex.c
arm/kernel/otp_stubs.c
arm/kernel/pm_stubs.c
arm/kernel/proc_a64.S
arm/kernel/ree_fs_ta.c
arm/kernel/spin_lock_debug.c
arm/kernel/tee_time_arm_cntpct.c
arm/kernel/tee_time_ree.c
arm/kernel/thread_a64.S
arm/kernel/tlb_helpers_a64.S
arm/kernel/trace_ext.c
arm/kernel/vfp.c
arm/kernel/vfp_a32.S
arm/kernel/vfp_a64.S
arm/kernel/vfp_private.h
arm/kernel/wait_queue.c
arm/mm/core_mmu_private.h
arm/mm/mobj.c
arm/mm/pgt_cache.c
arm/plat-d02/main.c
arm/plat-d02/platform_config.h
arm/plat-hikey/main.c
arm/plat-hikey/platform_config.h
arm/plat-hikey/spi_test.c
arm/plat-mediatek/main.c
arm/plat-mediatek/platform_config.h
arm/plat-rockchip/core_pos_a32.S
arm/plat-stm/platform_config.h
arm/plat-ti/main.c
arm/plat-ti/platform_config.h
arm/plat-vexpress/juno_core_pos_a64.S
arm/plat-vexpress/platform_config.h
arm/plat-vexpress/vendor_props.c
arm/pta/benchmark.c
arm/pta/core_fs_htree_tests.c
arm/pta/gprof.c
arm/pta/interrupt_tests.c
arm/pta/se_api_self_tests.c
arm/pta/stats.c
arm/tee/arch_svc.c
arm/tee/arch_svc_a64.S
arm/tee/arch_svc_private.h
arm/tee/pta_socket.c
arm/tee/svc_dummy.c
/optee_os/core/drivers/dra7_rng.c
/optee_os/core/drivers/hi16xx_rng.c
/optee_os/core/drivers/hi16xx_uart.c
/optee_os/core/drivers/pl011.c
/optee_os/core/drivers/pl022_spi.c
/optee_os/core/drivers/pl061_gpio.c
/optee_os/core/drivers/serial8250_uart.c
/optee_os/core/drivers/stih_asc.c
/optee_os/core/include/bench.h
/optee_os/core/include/console.h
/optee_os/core/include/crypto/crypto.h
/optee_os/core/include/crypto/internal_aes-gcm.h
/optee_os/core/include/drivers/hi16xx_uart.h
/optee_os/core/include/drivers/pl011.h
/optee_os/core/include/drivers/pl022_spi.h
/optee_os/core/include/drivers/pl061_gpio.h
/optee_os/core/include/drivers/serial.h
/optee_os/core/include/drivers/serial8250_uart.h
/optee_os/core/include/drivers/stih_asc.h
/optee_os/core/include/drivers/sunxi_uart.h
/optee_os/core/include/gpio.h
/optee_os/core/include/initcall.h
/optee_os/core/include/io.h
/optee_os/core/include/keep.h
/optee_os/core/include/kernel/asan.h
/optee_os/core/include/kernel/dt.h
/optee_os/core/include/kernel/handle.h
/optee_os/core/include/kernel/interrupt.h
/optee_os/core/include/kernel/trace_ta.h
/optee_os/core/include/optee_msg.h
/optee_os/core/include/optee_msg_supplicant.h
/optee_os/core/include/signed_hdr.h
/optee_os/core/include/spi.h
/optee_os/core/include/ta_pub_key.h
/optee_os/core/include/tee/cache.h
/optee_os/core/include/tee/fs_dirfile.h
/optee_os/core/include/tee/fs_htree.h
/optee_os/core/include/tee/se/aid.h
/optee_os/core/include/tee/se/apdu.h
/optee_os/core/include/tee/se/channel.h
/optee_os/core/include/tee/se/iso7816.h
/optee_os/core/include/tee/se/manager.h
/optee_os/core/include/tee/se/reader.h
/optee_os/core/include/tee/se/reader/interface.h
/optee_os/core/include/tee/se/service.h
/optee_os/core/include/tee/se/session.h
/optee_os/core/include/tee/se/svc.h
/optee_os/core/include/tee/se/util.h
/optee_os/core/include/tee/svc_cache.h
/optee_os/core/include/tee/tee_cryp_concat_kdf.h
/optee_os/core/include/tee/tee_cryp_hkdf.h
/optee_os/core/include/tee/tee_cryp_pbkdf2.h
/optee_os/core/include/tee/tee_cryp_utl.h
/optee_os/core/include/tee/tee_fs_key_manager.h
/optee_os/core/include/tee/tee_fs_rpc.h
/optee_os/core/include/tee/uuid.h
/optee_os/core/kernel/asan.c
/optee_os/core/kernel/console.c
/optee_os/core/kernel/dt.c
/optee_os/core/kernel/handle.c
/optee_os/core/kernel/interrupt.c
/optee_os/core/kernel/ubsan.c
/optee_os/core/lib/libtomcrypt/include/tomcrypt_arm_neon.h
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/tee_ltc_provider.c
/optee_os/core/tee/fs_dirfile.c
/optee_os/core/tee/fs_htree.c
/optee_os/core/tee/se/aid.c
/optee_os/core/tee/se/aid_priv.h
/optee_os/core/tee/se/apdu.c
/optee_os/core/tee/se/apdu_priv.h
/optee_os/core/tee/se/channel.c
/optee_os/core/tee/se/channel_priv.h
/optee_os/core/tee/se/iso7816.c
/optee_os/core/tee/se/manager.c
/optee_os/core/tee/se/reader.c
/optee_os/core/tee/se/reader/passthru_reader/driver.c
/optee_os/core/tee/se/reader/passthru_reader/pcsc.h
/optee_os/core/tee/se/reader/passthru_reader/reader.c
/optee_os/core/tee/se/reader/passthru_reader/reader.h
/optee_os/core/tee/se/reader_priv.h
/optee_os/core/tee/se/service.c
/optee_os/core/tee/se/service_priv.h
/optee_os/core/tee/se/session.c
/optee_os/core/tee/se/session_priv.h
/optee_os/core/tee/se/svc.c
/optee_os/core/tee/se/util.c
/optee_os/core/tee/tee_cryp_concat_kdf.c
/optee_os/core/tee/tee_cryp_hkdf.c
/optee_os/core/tee/tee_cryp_pbkdf2.c
/optee_os/core/tee/tee_cryp_utl.c
/optee_os/core/tee/tee_fs_key_manager.c
/optee_os/core/tee/tee_fs_rpc.c
/optee_os/core/tee/tee_fs_rpc_cache.c
/optee_os/core/tee/tee_ree_fs.c
/optee_os/core/tee/uuid.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_a32.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_a64.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.h
/optee_os/lib/libutee/arch/arm/utee_syscalls_a64.S
/optee_os/lib/libutee/include/__tee_ipsocket.h
/optee_os/lib/libutee/include/__tee_isocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines_extensions.h
/optee_os/lib/libutee/include/__tee_udpsocket_defines.h
/optee_os/lib/libutee/include/pta_benchmark.h
/optee_os/lib/libutee/include/pta_gprof.h
/optee_os/lib/libutee/include/pta_invoke_tests.h
/optee_os/lib/libutee/include/pta_socket.h
/optee_os/lib/libutee/include/tee_api_defines_extensions.h
/optee_os/lib/libutee/include/tee_internal_se_api.h
/optee_os/lib/libutee/include/tee_isocket.h
/optee_os/lib/libutee/include/tee_tcpsocket.h
/optee_os/lib/libutee/include/tee_udpsocket.h
/optee_os/lib/libutee/tee_api_private.h
/optee_os/lib/libutee/tee_api_se.c
/optee_os/lib/libutee/tee_socket_private.h
/optee_os/lib/libutee/tee_socket_pta.c
/optee_os/lib/libutee/tee_tcpudp_socket.c
/optee_os/lib/libutils/ext/arch/arm/aeabi_unwind.c
/optee_os/lib/libutils/ext/arch/arm/atomic_a32.S
/optee_os/lib/libutils/ext/arch/arm/atomic_a64.S
/optee_os/lib/libutils/ext/buf_compare_ct.c
/optee_os/lib/libutils/ext/include/printk.h
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_ldivmod_a32.S
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_shift.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_softfloat.c
/optee_os/lib/libutils/isoc/malloc_lock.c
/optee_os/lib/libutils/isoc/snprintf.c
/optee_os/scripts/gen_hashed_bin.py
/optee_os/scripts/gen_ld_sects.py
/optee_os/scripts/mem_usage.py
/optee_os/scripts/pem_to_pub_c.py
/optee_os/scripts/sign.py
/optee_os/scripts/symbolize.py
/optee_os/scripts/ta_bin_to_c.py
/optee_os/scripts/tee_bin_parser.py
78b7c7c715-Dec-2017 Jerome Forissier <jerome.forissier@linaro.org>

Remove license notice from Linaro files

Now that we have added SPDX identifiers, we can safely remove the
verbose license text from the files that are owned by Linaro.

Generated by [1]:
spdxify.p

Remove license notice from Linaro files

Now that we have added SPDX identifiers, we can safely remove the
verbose license text from the files that are owned by Linaro.

Generated by [1]:
spdxify.py --linaro-only --strip-license-text optee_os/

Link: [1] https://github.com/jforissier/misc/blob/f7b56c8/spdxify.py
Signed-off-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Joakim Bech <joakim.bech@linaro.org>

show more ...


arm/include/arm.h
arm/include/arm64.h
arm/include/arm64_macros.S
arm/include/kernel/abort.h
arm/include/kernel/cache_helpers.h
arm/include/kernel/early_ta.h
arm/include/kernel/generic_boot.h
arm/include/kernel/linker.h
arm/include/kernel/mutex.h
arm/include/kernel/pm_stubs.h
arm/include/kernel/pseudo_ta.h
arm/include/kernel/time_source.h
arm/include/kernel/user_ta.h
arm/include/kernel/vfp.h
arm/include/kernel/wait_queue.h
arm/include/mm/mobj.h
arm/include/mm/pgt_cache.h
arm/include/sm/optee_smc.h
arm/include/sm/teesmc_opteed.h
arm/include/sm/teesmc_opteed_macros.h
arm/include/tee/arch_svc.h
arm/kernel/abort.c
arm/kernel/asm-defines.c
arm/kernel/early_ta.c
arm/kernel/elf_load.c
arm/kernel/elf_load.h
arm/kernel/generic_boot.c
arm/kernel/generic_entry_a32.S
arm/kernel/generic_entry_a64.S
arm/kernel/link_dummies.c
arm/kernel/link_dummy.ld
arm/kernel/misc_a64.S
arm/kernel/mutex.c
arm/kernel/otp_stubs.c
arm/kernel/pm_stubs.c
arm/kernel/proc_a64.S
arm/kernel/ree_fs_ta.c
arm/kernel/spin_lock_debug.c
arm/kernel/tee_time_arm_cntpct.c
arm/kernel/tee_time_ree.c
arm/kernel/thread_a64.S
arm/kernel/tlb_helpers_a64.S
arm/kernel/trace_ext.c
arm/kernel/vfp.c
arm/kernel/vfp_a32.S
arm/kernel/vfp_a64.S
arm/kernel/vfp_private.h
arm/kernel/wait_queue.c
arm/mm/core_mmu_private.h
arm/mm/mobj.c
arm/mm/pgt_cache.c
arm/plat-d02/main.c
arm/plat-d02/platform_config.h
arm/plat-hikey/main.c
arm/plat-hikey/platform_config.h
arm/plat-hikey/spi_test.c
arm/plat-mediatek/main.c
arm/plat-mediatek/platform_config.h
arm/plat-rockchip/core_pos_a32.S
arm/plat-stm/platform_config.h
arm/plat-ti/main.c
arm/plat-ti/platform_config.h
arm/plat-vexpress/juno_core_pos_a64.S
arm/plat-vexpress/platform_config.h
arm/plat-vexpress/vendor_props.c
arm/pta/benchmark.c
arm/pta/core_fs_htree_tests.c
arm/pta/gprof.c
arm/pta/interrupt_tests.c
arm/pta/se_api_self_tests.c
arm/pta/stats.c
arm/tee/arch_svc.c
arm/tee/arch_svc_a64.S
arm/tee/arch_svc_private.h
arm/tee/pta_socket.c
arm/tee/svc_dummy.c
/optee_os/core/drivers/dra7_rng.c
/optee_os/core/drivers/hi16xx_rng.c
/optee_os/core/drivers/hi16xx_uart.c
/optee_os/core/drivers/pl011.c
/optee_os/core/drivers/pl022_spi.c
/optee_os/core/drivers/pl061_gpio.c
/optee_os/core/drivers/serial8250_uart.c
/optee_os/core/drivers/stih_asc.c
/optee_os/core/include/bench.h
/optee_os/core/include/console.h
/optee_os/core/include/crypto/crypto.h
/optee_os/core/include/drivers/hi16xx_uart.h
/optee_os/core/include/drivers/pl011.h
/optee_os/core/include/drivers/pl022_spi.h
/optee_os/core/include/drivers/pl061_gpio.h
/optee_os/core/include/drivers/serial.h
/optee_os/core/include/drivers/serial8250_uart.h
/optee_os/core/include/drivers/stih_asc.h
/optee_os/core/include/drivers/sunxi_uart.h
/optee_os/core/include/gpio.h
/optee_os/core/include/initcall.h
/optee_os/core/include/io.h
/optee_os/core/include/keep.h
/optee_os/core/include/kernel/asan.h
/optee_os/core/include/kernel/dt.h
/optee_os/core/include/kernel/handle.h
/optee_os/core/include/kernel/interrupt.h
/optee_os/core/include/kernel/trace_ta.h
/optee_os/core/include/optee_msg.h
/optee_os/core/include/optee_msg_supplicant.h
/optee_os/core/include/signed_hdr.h
/optee_os/core/include/spi.h
/optee_os/core/include/ta_pub_key.h
/optee_os/core/include/tee/cache.h
/optee_os/core/include/tee/fs_dirfile.h
/optee_os/core/include/tee/fs_htree.h
/optee_os/core/include/tee/se/aid.h
/optee_os/core/include/tee/se/apdu.h
/optee_os/core/include/tee/se/channel.h
/optee_os/core/include/tee/se/iso7816.h
/optee_os/core/include/tee/se/manager.h
/optee_os/core/include/tee/se/reader.h
/optee_os/core/include/tee/se/reader/interface.h
/optee_os/core/include/tee/se/service.h
/optee_os/core/include/tee/se/session.h
/optee_os/core/include/tee/se/svc.h
/optee_os/core/include/tee/se/util.h
/optee_os/core/include/tee/svc_cache.h
/optee_os/core/include/tee/tee_cryp_concat_kdf.h
/optee_os/core/include/tee/tee_cryp_hkdf.h
/optee_os/core/include/tee/tee_cryp_pbkdf2.h
/optee_os/core/include/tee/tee_cryp_utl.h
/optee_os/core/include/tee/tee_fs_key_manager.h
/optee_os/core/include/tee/tee_fs_rpc.h
/optee_os/core/include/tee/uuid.h
/optee_os/core/kernel/asan.c
/optee_os/core/kernel/console.c
/optee_os/core/kernel/dt.c
/optee_os/core/kernel/handle.c
/optee_os/core/kernel/interrupt.c
/optee_os/core/kernel/ubsan.c
/optee_os/core/lib/libtomcrypt/include/tomcrypt_arm_neon.h
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/tee_ltc_provider.c
/optee_os/core/tee/fs_dirfile.c
/optee_os/core/tee/fs_htree.c
/optee_os/core/tee/se/aid.c
/optee_os/core/tee/se/aid_priv.h
/optee_os/core/tee/se/apdu.c
/optee_os/core/tee/se/apdu_priv.h
/optee_os/core/tee/se/channel.c
/optee_os/core/tee/se/channel_priv.h
/optee_os/core/tee/se/iso7816.c
/optee_os/core/tee/se/manager.c
/optee_os/core/tee/se/reader.c
/optee_os/core/tee/se/reader/passthru_reader/driver.c
/optee_os/core/tee/se/reader/passthru_reader/pcsc.h
/optee_os/core/tee/se/reader/passthru_reader/reader.c
/optee_os/core/tee/se/reader/passthru_reader/reader.h
/optee_os/core/tee/se/reader_priv.h
/optee_os/core/tee/se/service.c
/optee_os/core/tee/se/service_priv.h
/optee_os/core/tee/se/session.c
/optee_os/core/tee/se/session_priv.h
/optee_os/core/tee/se/svc.c
/optee_os/core/tee/se/util.c
/optee_os/core/tee/tee_cryp_concat_kdf.c
/optee_os/core/tee/tee_cryp_hkdf.c
/optee_os/core/tee/tee_cryp_pbkdf2.c
/optee_os/core/tee/tee_cryp_utl.c
/optee_os/core/tee/tee_fs_key_manager.c
/optee_os/core/tee/tee_fs_rpc.c
/optee_os/core/tee/tee_fs_rpc_cache.c
/optee_os/core/tee/tee_ree_fs.c
/optee_os/core/tee/uuid.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_a32.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_a64.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.h
/optee_os/lib/libutee/arch/arm/utee_syscalls_a64.S
/optee_os/lib/libutee/include/__tee_ipsocket.h
/optee_os/lib/libutee/include/__tee_isocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines_extensions.h
/optee_os/lib/libutee/include/__tee_udpsocket_defines.h
/optee_os/lib/libutee/include/pta_benchmark.h
/optee_os/lib/libutee/include/pta_gprof.h
/optee_os/lib/libutee/include/pta_invoke_tests.h
/optee_os/lib/libutee/include/pta_socket.h
/optee_os/lib/libutee/include/tee_api_defines_extensions.h
/optee_os/lib/libutee/include/tee_internal_se_api.h
/optee_os/lib/libutee/include/tee_isocket.h
/optee_os/lib/libutee/include/tee_tcpsocket.h
/optee_os/lib/libutee/include/tee_udpsocket.h
/optee_os/lib/libutee/tee_api_private.h
/optee_os/lib/libutee/tee_api_se.c
/optee_os/lib/libutee/tee_socket_private.h
/optee_os/lib/libutee/tee_socket_pta.c
/optee_os/lib/libutee/tee_tcpudp_socket.c
/optee_os/lib/libutils/ext/arch/arm/aeabi_unwind.c
/optee_os/lib/libutils/ext/arch/arm/atomic_a32.S
/optee_os/lib/libutils/ext/arch/arm/atomic_a64.S
/optee_os/lib/libutils/ext/buf_compare_ct.c
/optee_os/lib/libutils/ext/include/printk.h
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_ldivmod_a32.S
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_shift.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_softfloat.c
/optee_os/lib/libutils/isoc/malloc_lock.c
/optee_os/lib/libutils/isoc/snprintf.c
/optee_os/scripts/gen_hashed_bin.py
/optee_os/scripts/gen_ld_sects.py
/optee_os/scripts/pem_to_pub_c.py
/optee_os/scripts/sign.py
/optee_os/scripts/symbolize.py
/optee_os/scripts/ta_bin_to_c.py
/optee_os/scripts/tee_bin_parser.py
1bb9298315-Dec-2017 Jerome Forissier <jerome.forissier@linaro.org>

Add SPDX license identifiers

Adds one SPDX-License-Identifier line [1] to each source files that
contains license text.

Generated by [2]:
spdxify.py --add-spdx optee_os/

The scancode tool [3] wa

Add SPDX license identifiers

Adds one SPDX-License-Identifier line [1] to each source files that
contains license text.

Generated by [2]:
spdxify.py --add-spdx optee_os/

The scancode tool [3] was used to double check the license matching
code in the Python script. All the licenses detected by scancode are
either detected by spdxify.py, or have no SPDX identifier, or are false
matches.

Link: [1] https://spdx.org/licenses/
Link: [2] https://github.com/jforissier/misc/blob/f7b56c8/spdxify.py
Link: [3] https://github.com/nexB/scancode-toolkit
Signed-off-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Joakim Bech <joakim.bech@linaro.org>

show more ...


arm/include/arm.h
arm/include/arm32.h
arm/include/arm32_macros.S
arm/include/arm32_macros_cortex_a9.S
arm/include/arm64.h
arm/include/arm64_macros.S
arm/include/kernel/abort.h
arm/include/kernel/cache_helpers.h
arm/include/kernel/delay.h
arm/include/kernel/early_ta.h
arm/include/kernel/generic_boot.h
arm/include/kernel/linker.h
arm/include/kernel/misc.h
arm/include/kernel/mutex.h
arm/include/kernel/pm_stubs.h
arm/include/kernel/pseudo_ta.h
arm/include/kernel/spinlock.h
arm/include/kernel/tee_l2cc_mutex.h
arm/include/kernel/thread.h
arm/include/kernel/thread_defs.h
arm/include/kernel/time_source.h
arm/include/kernel/tlb_helpers.h
arm/include/kernel/tz_proc_def.h
arm/include/kernel/tz_ssvce_def.h
arm/include/kernel/tz_ssvce_pl310.h
arm/include/kernel/user_ta.h
arm/include/kernel/vfp.h
arm/include/kernel/wait_queue.h
arm/include/mm/core_memprot.h
arm/include/mm/core_mmu.h
arm/include/mm/mobj.h
arm/include/mm/pgt_cache.h
arm/include/mm/tee_pager.h
arm/include/sm/optee_smc.h
arm/include/sm/pm.h
arm/include/sm/sm.h
arm/include/sm/tee_mon.h
arm/include/sm/teesmc_opteed.h
arm/include/sm/teesmc_opteed_macros.h
arm/include/tee/arch_svc.h
arm/include/tee/entry_fast.h
arm/include/tee/entry_std.h
arm/kernel/abort.c
arm/kernel/asm-defines.c
arm/kernel/delay.c
arm/kernel/early_ta.c
arm/kernel/elf32.h
arm/kernel/elf64.h
arm/kernel/elf_common.h
arm/kernel/elf_load.c
arm/kernel/elf_load.h
arm/kernel/generic_boot.c
arm/kernel/generic_entry_a32.S
arm/kernel/generic_entry_a64.S
arm/kernel/kern.ld.S
arm/kernel/link_dummies.c
arm/kernel/link_dummy.ld
arm/kernel/misc_a32.S
arm/kernel/misc_a64.S
arm/kernel/mutex.c
arm/kernel/otp_stubs.c
arm/kernel/pm_stubs.c
arm/kernel/proc_a32.S
arm/kernel/proc_a64.S
arm/kernel/pseudo_ta.c
arm/kernel/ree_fs_ta.c
arm/kernel/spin_lock_a32.S
arm/kernel/spin_lock_a64.S
arm/kernel/spin_lock_debug.c
arm/kernel/tee_l2cc_mutex.c
arm/kernel/tee_time.c
arm/kernel/tee_time_arm_cntpct.c
arm/kernel/tee_time_ree.c
arm/kernel/thread.c
arm/kernel/thread_a32.S
arm/kernel/thread_a64.S
arm/kernel/thread_private.h
arm/kernel/tlb_helpers_a32.S
arm/kernel/tlb_helpers_a64.S
arm/kernel/trace_ext.c
arm/kernel/tz_ssvce_pl310_a32.S
arm/kernel/unwind_arm32.c
arm/kernel/unwind_arm64.c
arm/kernel/user_ta.c
arm/kernel/vfp.c
arm/kernel/vfp_a32.S
arm/kernel/vfp_a64.S
arm/kernel/vfp_private.h
arm/kernel/wait_queue.c
arm/mm/core_mmu.c
arm/mm/core_mmu_lpae.c
arm/mm/core_mmu_private.h
arm/mm/core_mmu_v7.c
arm/mm/mobj.c
arm/mm/pgt_cache.c
arm/mm/tee_mm.c
arm/mm/tee_mmu.c
arm/mm/tee_pager.c
arm/plat-d02/main.c
arm/plat-d02/platform_config.h
arm/plat-hikey/hikey_peripherals.h
arm/plat-hikey/main.c
arm/plat-hikey/platform_config.h
arm/plat-hikey/spi_test.c
arm/plat-imx/a7_plat_init.S
arm/plat-imx/a9_plat_init.S
arm/plat-imx/config/config_imx6sx.h
arm/plat-imx/config/config_imx7.h
arm/plat-imx/imx-common.c
arm/plat-imx/imx-regs.h
arm/plat-imx/imx.h
arm/plat-imx/imx6.c
arm/plat-imx/imx6ul.c
arm/plat-imx/imx7.c
arm/plat-imx/imx_pl310.c
arm/plat-imx/imx_pm.h
arm/plat-imx/main.c
arm/plat-imx/mmdc.c
arm/plat-imx/mmdc.h
arm/plat-imx/platform_config.h
arm/plat-imx/pm/gpcv2.c
arm/plat-imx/pm/imx7_suspend.c
arm/plat-imx/pm/pm-imx7.c
arm/plat-imx/pm/psci-suspend-imx7.S
arm/plat-imx/pm/psci.c
arm/plat-ls/ls_core_pos_a32.S
arm/plat-ls/ls_core_pos_a64.S
arm/plat-ls/main.c
arm/plat-ls/plat_init.S
arm/plat-ls/platform_config.h
arm/plat-marvell/armada3700/hal_sec_perf.c
arm/plat-marvell/armada7k8k/hal_sec_perf.c
arm/plat-marvell/main.c
arm/plat-marvell/platform_config.h
arm/plat-mediatek/main.c
arm/plat-mediatek/platform_config.h
arm/plat-rcar/main.c
arm/plat-rcar/platform_config.h
arm/plat-rockchip/common.h
arm/plat-rockchip/core_pos_a32.S
arm/plat-rockchip/cru.h
arm/plat-rockchip/grf.h
arm/plat-rockchip/main.c
arm/plat-rockchip/plat_init.S
arm/plat-rockchip/platform.c
arm/plat-rockchip/platform_config.h
arm/plat-rockchip/psci_rk322x.c
arm/plat-rpi3/main.c
arm/plat-rpi3/platform_config.h
arm/plat-sam/main.c
arm/plat-sam/matrix.c
arm/plat-sam/matrix.h
arm/plat-sam/platform_config.h
arm/plat-sam/sama5d2.h
arm/plat-sam/tz_matrix.h
arm/plat-sprd/console.c
arm/plat-sprd/main.c
arm/plat-sprd/platform_config.h
arm/plat-stm/main.c
arm/plat-stm/platform_config.h
arm/plat-stm/rng_support.c
arm/plat-stm/tz_a9init.S
arm/plat-sunxi/entry.S
arm/plat-sunxi/head.c
arm/plat-sunxi/kern.ld.S
arm/plat-sunxi/main.c
arm/plat-sunxi/platform.c
arm/plat-sunxi/platform.h
arm/plat-sunxi/platform_config.h
arm/plat-sunxi/rng_support.c
arm/plat-sunxi/smp_boot.S
arm/plat-sunxi/smp_fixup.S
arm/plat-ti/a9_plat_init.S
arm/plat-ti/api_monitor_index_a15.h
arm/plat-ti/api_monitor_index_a9.h
arm/plat-ti/main.c
arm/plat-ti/platform_config.h
arm/plat-ti/sm_platform_handler_a15.c
arm/plat-ti/sm_platform_handler_a9.c
arm/plat-ti/ti_pl310.c
arm/plat-vexpress/juno_core_pos_a32.S
arm/plat-vexpress/juno_core_pos_a64.S
arm/plat-vexpress/main.c
arm/plat-vexpress/platform_config.h
arm/plat-vexpress/vendor_props.c
arm/plat-zynq7k/main.c
arm/plat-zynq7k/plat_init.S
arm/plat-zynq7k/platform_config.h
arm/plat-zynq7k/platform_smc.h
arm/plat-zynqmp/main.c
arm/plat-zynqmp/platform_config.h
arm/pta/benchmark.c
arm/pta/core_fs_htree_tests.c
arm/pta/core_self_tests.c
arm/pta/core_self_tests.h
arm/pta/gprof.c
arm/pta/interrupt_tests.c
arm/pta/pta_invoke_tests.c
arm/pta/se_api_self_tests.c
arm/pta/stats.c
arm/sm/pm.c
arm/sm/pm_a32.S
arm/sm/psci-helper.S
arm/sm/psci.c
arm/sm/sm.c
arm/sm/sm_a32.S
arm/sm/sm_private.h
arm/sm/std_smc.c
arm/tee/arch_svc.c
arm/tee/arch_svc_a32.S
arm/tee/arch_svc_a64.S
arm/tee/arch_svc_private.h
arm/tee/cache.c
arm/tee/entry_fast.c
arm/tee/entry_std.c
arm/tee/init.c
arm/tee/pta_socket.c
arm/tee/svc_cache.c
arm/tee/svc_dummy.c
/optee_os/core/crypto/aes-gcm-ghash.c
/optee_os/core/drivers/atmel_uart.c
/optee_os/core/drivers/cdns_uart.c
/optee_os/core/drivers/dra7_rng.c
/optee_os/core/drivers/gic.c
/optee_os/core/drivers/hi16xx_rng.c
/optee_os/core/drivers/hi16xx_uart.c
/optee_os/core/drivers/imx_snvs.c
/optee_os/core/drivers/imx_uart.c
/optee_os/core/drivers/imx_wdog.c
/optee_os/core/drivers/mvebu_uart.c
/optee_os/core/drivers/ns16550.c
/optee_os/core/drivers/pl011.c
/optee_os/core/drivers/pl022_spi.c
/optee_os/core/drivers/pl061_gpio.c
/optee_os/core/drivers/scif.c
/optee_os/core/drivers/serial8250_uart.c
/optee_os/core/drivers/sprd_uart.c
/optee_os/core/drivers/stih_asc.c
/optee_os/core/drivers/sunxi_uart.c
/optee_os/core/drivers/tzc380.c
/optee_os/core/drivers/tzc400.c
/optee_os/core/include/bench.h
/optee_os/core/include/console.h
/optee_os/core/include/crypto/crypto.h
/optee_os/core/include/drivers/atmel_uart.h
/optee_os/core/include/drivers/cdns_uart.h
/optee_os/core/include/drivers/gic.h
/optee_os/core/include/drivers/hi16xx_uart.h
/optee_os/core/include/drivers/imx_snvs.h
/optee_os/core/include/drivers/imx_uart.h
/optee_os/core/include/drivers/imx_wdog.h
/optee_os/core/include/drivers/mvebu_uart.h
/optee_os/core/include/drivers/ns16550.h
/optee_os/core/include/drivers/pl011.h
/optee_os/core/include/drivers/pl022_spi.h
/optee_os/core/include/drivers/pl061_gpio.h
/optee_os/core/include/drivers/scif.h
/optee_os/core/include/drivers/serial.h
/optee_os/core/include/drivers/serial8250_uart.h
/optee_os/core/include/drivers/sprd_uart.h
/optee_os/core/include/drivers/stih_asc.h
/optee_os/core/include/drivers/sunxi_uart.h
/optee_os/core/include/drivers/tzc380.h
/optee_os/core/include/drivers/tzc400.h
/optee_os/core/include/gpio.h
/optee_os/core/include/initcall.h
/optee_os/core/include/io.h
/optee_os/core/include/keep.h
/optee_os/core/include/kernel/asan.h
/optee_os/core/include/kernel/chip_services.h
/optee_os/core/include/kernel/dt.h
/optee_os/core/include/kernel/handle.h
/optee_os/core/include/kernel/interrupt.h
/optee_os/core/include/kernel/msg_param.h
/optee_os/core/include/kernel/panic.h
/optee_os/core/include/kernel/tee_common.h
/optee_os/core/include/kernel/tee_common_otp.h
/optee_os/core/include/kernel/tee_customer_part.h
/optee_os/core/include/kernel/tee_kta_trace.h
/optee_os/core/include/kernel/tee_misc.h
/optee_os/core/include/kernel/tee_ta_manager.h
/optee_os/core/include/kernel/tee_time.h
/optee_os/core/include/kernel/trace_ta.h
/optee_os/core/include/mm/tee_mm.h
/optee_os/core/include/mm/tee_mmu.h
/optee_os/core/include/mm/tee_mmu_types.h
/optee_os/core/include/optee_msg.h
/optee_os/core/include/optee_msg_supplicant.h
/optee_os/core/include/rng_support.h
/optee_os/core/include/signed_hdr.h
/optee_os/core/include/spi.h
/optee_os/core/include/ta_pub_key.h
/optee_os/core/include/tee/cache.h
/optee_os/core/include/tee/fs_dirfile.h
/optee_os/core/include/tee/fs_htree.h
/optee_os/core/include/tee/se/aid.h
/optee_os/core/include/tee/se/apdu.h
/optee_os/core/include/tee/se/channel.h
/optee_os/core/include/tee/se/iso7816.h
/optee_os/core/include/tee/se/manager.h
/optee_os/core/include/tee/se/reader.h
/optee_os/core/include/tee/se/reader/interface.h
/optee_os/core/include/tee/se/service.h
/optee_os/core/include/tee/se/session.h
/optee_os/core/include/tee/se/svc.h
/optee_os/core/include/tee/se/util.h
/optee_os/core/include/tee/svc_cache.h
/optee_os/core/include/tee/tee_cryp_concat_kdf.h
/optee_os/core/include/tee/tee_cryp_hkdf.h
/optee_os/core/include/tee/tee_cryp_pbkdf2.h
/optee_os/core/include/tee/tee_cryp_utl.h
/optee_os/core/include/tee/tee_fs.h
/optee_os/core/include/tee/tee_fs_key_manager.h
/optee_os/core/include/tee/tee_fs_rpc.h
/optee_os/core/include/tee/tee_obj.h
/optee_os/core/include/tee/tee_pobj.h
/optee_os/core/include/tee/tee_svc.h
/optee_os/core/include/tee/tee_svc_cryp.h
/optee_os/core/include/tee/tee_svc_storage.h
/optee_os/core/include/tee/uuid.h
/optee_os/core/kernel/asan.c
/optee_os/core/kernel/assert.c
/optee_os/core/kernel/console.c
/optee_os/core/kernel/dt.c
/optee_os/core/kernel/handle.c
/optee_os/core/kernel/interrupt.c
/optee_os/core/kernel/msg_param.c
/optee_os/core/kernel/panic.c
/optee_os/core/kernel/tee_misc.c
/optee_os/core/kernel/tee_ta_manager.c
/optee_os/core/kernel/ubsan.c
/optee_os/core/lib/libfdt/fdt.c
/optee_os/core/lib/libfdt/fdt_addresses.c
/optee_os/core/lib/libfdt/fdt_empty_tree.c
/optee_os/core/lib/libfdt/fdt_ro.c
/optee_os/core/lib/libfdt/fdt_rw.c
/optee_os/core/lib/libfdt/fdt_strerror.c
/optee_os/core/lib/libfdt/fdt_sw.c
/optee_os/core/lib/libfdt/fdt_wip.c
/optee_os/core/lib/libfdt/include/fdt.h
/optee_os/core/lib/libfdt/include/libfdt.h
/optee_os/core/lib/libfdt/include/libfdt_env.h
/optee_os/core/lib/libfdt/libfdt_internal.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_argchk.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_arm_neon.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_cfg.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_cipher.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_custom.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_hash.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_mac.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_macros.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_math.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_misc.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_mpa.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_pk.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_pkcs.h
/optee_os/core/lib/libtomcrypt/include/tomcrypt_prng.h
/optee_os/core/lib/libtomcrypt/src/ciphers/aes.c
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_armv8a_ce.c
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_modes_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/ciphers/aes_tab.c
/optee_os/core/lib/libtomcrypt/src/ciphers/des.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_add_aad.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_add_nonce.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_done.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_init.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_process.c
/optee_os/core/lib/libtomcrypt/src/encauth/ccm/ccm_reset.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_addheader.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_decrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_decrypt_verify_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_done.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_encrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_encrypt_authenticate_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/eax/eax_init.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_add_aad.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_add_iv.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_done.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_gf_mult.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_init.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_mult_h.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_process.c
/optee_os/core/lib/libtomcrypt/src/encauth/gcm/gcm_reset.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_decrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_decrypt_verify_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_done_decrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_done_encrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_encrypt.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_encrypt_authenticate_memory.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_init.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_ntz.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/ocb_shift_xor.c
/optee_os/core/lib/libtomcrypt/src/encauth/ocb/s_ocb_done.c
/optee_os/core/lib/libtomcrypt/src/hashes/helper/hash_file.c
/optee_os/core/lib/libtomcrypt/src/hashes/helper/hash_filehandle.c
/optee_os/core/lib/libtomcrypt/src/hashes/helper/hash_memory.c
/optee_os/core/lib/libtomcrypt/src/hashes/helper/hash_memory_multi.c
/optee_os/core/lib/libtomcrypt/src/hashes/md5.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha1.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha1_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha224.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a32.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha256_armv8a_ce_a64.S
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha384.c
/optee_os/core/lib/libtomcrypt/src/hashes/sha2/sha512.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_done.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_file.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_init.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_memory.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_memory_multi.c
/optee_os/core/lib/libtomcrypt/src/mac/hmac/hmac_process.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_done.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_file.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_init.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_memory.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_memory_multi.c
/optee_os/core/lib/libtomcrypt/src/mac/omac/omac_process.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_done.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_file.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_init.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_memory.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_memory_multi.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_ntz.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_process.c
/optee_os/core/lib/libtomcrypt/src/mac/pmac/pmac_shift_xor.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_done.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_file.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_init.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_memory.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_memory_multi.c
/optee_os/core/lib/libtomcrypt/src/mac/xcbc/xcbc_process.c
/optee_os/core/lib/libtomcrypt/src/math/fp/ltc_ecc_fp_mulmod.c
/optee_os/core/lib/libtomcrypt/src/math/multi.c
/optee_os/core/lib/libtomcrypt/src/math/rand_prime.c
/optee_os/core/lib/libtomcrypt/src/misc/base64/base64_decode.c
/optee_os/core/lib/libtomcrypt/src/misc/base64/base64_encode.c
/optee_os/core/lib/libtomcrypt/src/misc/burn_stack.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_argchk.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_cipher_descriptor.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_cipher_is_valid.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_cipher.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_cipher_any.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_cipher_id.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_hash.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_hash_any.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_hash_id.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_hash_oid.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_find_prng.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_fsa.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_hash_descriptor.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_hash_is_valid.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_prng_descriptor.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_prng_is_valid.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_register_cipher.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_register_hash.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_register_prng.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_unregister_cipher.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_unregister_hash.c
/optee_os/core/lib/libtomcrypt/src/misc/crypt/crypt_unregister_prng.c
/optee_os/core/lib/libtomcrypt/src/misc/error_to_string.c
/optee_os/core/lib/libtomcrypt/src/misc/mem_neq.c
/optee_os/core/lib/libtomcrypt/src/misc/pkcs5/pkcs_5_1.c
/optee_os/core/lib/libtomcrypt/src/misc/pkcs5/pkcs_5_2.c
/optee_os/core/lib/libtomcrypt/src/misc/zeromem.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_done.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/cbc/cbc_start.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_done.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/cfb/cfb_start.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_done.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/ctr/ctr_start.c
/optee_os/core/lib/libtomcrypt/src/modes/ecb/ecb_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ecb/ecb_done.c
/optee_os/core/lib/libtomcrypt/src/modes/ecb/ecb_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ecb/ecb_start.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_done.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/f8/f8_start.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_done.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_process.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/lrw/lrw_start.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_done.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_getiv.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_setiv.c
/optee_os/core/lib/libtomcrypt/src/modes/ofb/ofb_start.c
/optee_os/core/lib/libtomcrypt/src/modes/xts/xts_decrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/xts/xts_done.c
/optee_os/core/lib/libtomcrypt/src/modes/xts/xts_encrypt.c
/optee_os/core/lib/libtomcrypt/src/modes/xts/xts_init.c
/optee_os/core/lib/libtomcrypt/src/modes/xts/xts_mult_x.c
/optee_os/core/lib/libtomcrypt/src/mpa_desc.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/bit/der_decode_bit_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/bit/der_decode_raw_bit_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/bit/der_encode_bit_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/bit/der_encode_raw_bit_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/bit/der_length_bit_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/boolean/der_decode_boolean.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/boolean/der_encode_boolean.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/boolean/der_length_boolean.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/choice/der_decode_choice.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/ia5/der_decode_ia5_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/ia5/der_encode_ia5_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/ia5/der_length_ia5_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/integer/der_decode_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/integer/der_encode_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/integer/der_length_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_decode_object_identifier.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_encode_object_identifier.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/object_identifier/der_length_object_identifier.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/octet/der_decode_octet_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/octet/der_encode_octet_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/octet/der_length_octet_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/printable_string/der_decode_printable_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/printable_string/der_encode_printable_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/printable_string/der_length_printable_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_ex.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_flexi.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_sequence_multi.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_decode_subject_public_key_info.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_encode_sequence_ex.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_encode_sequence_multi.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_encode_subject_public_key_info.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_length_sequence.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/sequence/der_sequence_free.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/set/der_encode_set.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/set/der_encode_setof.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/short_integer/der_decode_short_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/short_integer/der_encode_short_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/short_integer/der_length_short_integer.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/teletex_string/der_decode_teletex_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/teletex_string/der_length_teletex_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utctime/der_decode_utctime.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utctime/der_encode_utctime.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utctime/der_length_utctime.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utf8/der_decode_utf8_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utf8/der_encode_utf8_string.c
/optee_os/core/lib/libtomcrypt/src/pk/asn1/der/utf8/der_length_utf8_string.c
/optee_os/core/lib/libtomcrypt/src/pk/dh/dh.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_decrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_encrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_export.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_free.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_import.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_make_key.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_shared_secret.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_sign_hash.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_verify_hash.c
/optee_os/core/lib/libtomcrypt/src/pk/dsa/dsa_verify_key.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_ansi_x963_export.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_ansi_x963_import.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_decrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_encrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_export.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_free.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_get_size.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_import.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_make_key.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_shared_secret.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_sign_hash.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_sizes.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ecc_verify_hash.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_is_valid_idx.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_map.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_mul2add.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_mulmod.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_mulmod_timing.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_points.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_projective_add_point.c
/optee_os/core/lib/libtomcrypt/src/pk/ecc/ltc_ecc_projective_dbl_point.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_i2osp.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_mgf1.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_oaep_decode.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_oaep_encode.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_os2ip.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_pss_decode.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_pss_encode.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_v1_5_decode.c
/optee_os/core/lib/libtomcrypt/src/pk/pkcs1/pkcs_1_v1_5_encode.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_decrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_encrypt_key.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_export.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_exptmod.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_free.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_import.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_make_key.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_sign_hash.c
/optee_os/core/lib/libtomcrypt/src/pk/rsa/rsa_verify_hash.c
/optee_os/core/lib/libtomcrypt/src/prngs/rng_get_bytes.c
/optee_os/core/lib/libtomcrypt/src/prngs/rng_make_prng.c
/optee_os/core/lib/libtomcrypt/src/prngs/sprng.c
/optee_os/core/lib/libtomcrypt/src/prngs/yarrow.c
/optee_os/core/lib/libtomcrypt/src/tee_ltc_provider.c
/optee_os/core/lib/zlib/adler32.c
/optee_os/core/lib/zlib/gzguts.h
/optee_os/core/lib/zlib/inffast.c
/optee_os/core/lib/zlib/inffast.h
/optee_os/core/lib/zlib/inflate.c
/optee_os/core/lib/zlib/inflate.h
/optee_os/core/lib/zlib/inftrees.c
/optee_os/core/lib/zlib/inftrees.h
/optee_os/core/lib/zlib/zconf.h
/optee_os/core/lib/zlib/zlib.h
/optee_os/core/lib/zlib/zutil.c
/optee_os/core/lib/zlib/zutil.h
/optee_os/core/tee/fs_dirfile.c
/optee_os/core/tee/fs_htree.c
/optee_os/core/tee/se/aid.c
/optee_os/core/tee/se/aid_priv.h
/optee_os/core/tee/se/apdu.c
/optee_os/core/tee/se/apdu_priv.h
/optee_os/core/tee/se/channel.c
/optee_os/core/tee/se/channel_priv.h
/optee_os/core/tee/se/iso7816.c
/optee_os/core/tee/se/manager.c
/optee_os/core/tee/se/reader.c
/optee_os/core/tee/se/reader/passthru_reader/driver.c
/optee_os/core/tee/se/reader/passthru_reader/pcsc.h
/optee_os/core/tee/se/reader/passthru_reader/reader.c
/optee_os/core/tee/se/reader/passthru_reader/reader.h
/optee_os/core/tee/se/reader_priv.h
/optee_os/core/tee/se/service.c
/optee_os/core/tee/se/service_priv.h
/optee_os/core/tee/se/session.c
/optee_os/core/tee/se/session_priv.h
/optee_os/core/tee/se/svc.c
/optee_os/core/tee/se/util.c
/optee_os/core/tee/tee_cryp_concat_kdf.c
/optee_os/core/tee/tee_cryp_hkdf.c
/optee_os/core/tee/tee_cryp_pbkdf2.c
/optee_os/core/tee/tee_cryp_utl.c
/optee_os/core/tee/tee_fs_key_manager.c
/optee_os/core/tee/tee_fs_rpc.c
/optee_os/core/tee/tee_fs_rpc_cache.c
/optee_os/core/tee/tee_obj.c
/optee_os/core/tee/tee_pobj.c
/optee_os/core/tee/tee_ree_fs.c
/optee_os/core/tee/tee_rpmb_fs.c
/optee_os/core/tee/tee_svc.c
/optee_os/core/tee/tee_svc_cryp.c
/optee_os/core/tee/tee_svc_storage.c
/optee_os/core/tee/tee_time_generic.c
/optee_os/core/tee/uuid.c
/optee_os/lib/libmpa/arch/arm/mpa_a32.S
/optee_os/lib/libmpa/include/mpa.h
/optee_os/lib/libmpa/include/mpalib.h
/optee_os/lib/libmpa/include/mpalib_config.h
/optee_os/lib/libmpa/mpa_addsub.c
/optee_os/lib/libmpa/mpa_cmp.c
/optee_os/lib/libmpa/mpa_conv.c
/optee_os/lib/libmpa/mpa_div.c
/optee_os/lib/libmpa/mpa_expmod.c
/optee_os/lib/libmpa/mpa_gcd.c
/optee_os/lib/libmpa/mpa_init.c
/optee_os/lib/libmpa/mpa_io.c
/optee_os/lib/libmpa/mpa_mem_static.c
/optee_os/lib/libmpa/mpa_misc.c
/optee_os/lib/libmpa/mpa_modulus.c
/optee_os/lib/libmpa/mpa_montgomery.c
/optee_os/lib/libmpa/mpa_mul.c
/optee_os/lib/libmpa/mpa_primetable.h
/optee_os/lib/libmpa/mpa_primetest.c
/optee_os/lib/libmpa/mpa_random.c
/optee_os/lib/libmpa/mpa_shift.c
/optee_os/lib/libutee/abort.c
/optee_os/lib/libutee/arch/arm/gprof/gmon.h
/optee_os/lib/libutee/arch/arm/gprof/gmon_out.h
/optee_os/lib/libutee/arch/arm/gprof/gprof.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_a32.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_a64.S
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.c
/optee_os/lib/libutee/arch/arm/gprof/gprof_pta.h
/optee_os/lib/libutee/arch/arm/user_ta_entry.c
/optee_os/lib/libutee/arch/arm/utee_misc.c
/optee_os/lib/libutee/arch/arm/utee_syscalls_a32.S
/optee_os/lib/libutee/arch/arm/utee_syscalls_a64.S
/optee_os/lib/libutee/arch/arm/utee_syscalls_asm.S
/optee_os/lib/libutee/assert.c
/optee_os/lib/libutee/base64.c
/optee_os/lib/libutee/base64.h
/optee_os/lib/libutee/errno.c
/optee_os/lib/libutee/include/__tee_ipsocket.h
/optee_os/lib/libutee/include/__tee_isocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines.h
/optee_os/lib/libutee/include/__tee_tcpsocket_defines_extensions.h
/optee_os/lib/libutee/include/__tee_udpsocket_defines.h
/optee_os/lib/libutee/include/pta_benchmark.h
/optee_os/lib/libutee/include/pta_gprof.h
/optee_os/lib/libutee/include/pta_invoke_tests.h
/optee_os/lib/libutee/include/pta_socket.h
/optee_os/lib/libutee/include/tee_api.h
/optee_os/lib/libutee/include/tee_api_defines.h
/optee_os/lib/libutee/include/tee_api_defines_extensions.h
/optee_os/lib/libutee/include/tee_api_types.h
/optee_os/lib/libutee/include/tee_arith_internal.h
/optee_os/lib/libutee/include/tee_internal_api.h
/optee_os/lib/libutee/include/tee_internal_api_extensions.h
/optee_os/lib/libutee/include/tee_internal_se_api.h
/optee_os/lib/libutee/include/tee_isocket.h
/optee_os/lib/libutee/include/tee_syscall_numbers.h
/optee_os/lib/libutee/include/tee_ta_api.h
/optee_os/lib/libutee/include/tee_tcpsocket.h
/optee_os/lib/libutee/include/tee_udpsocket.h
/optee_os/lib/libutee/include/user_ta_header.h
/optee_os/lib/libutee/include/utee_defines.h
/optee_os/lib/libutee/include/utee_syscalls.h
/optee_os/lib/libutee/include/utee_types.h
/optee_os/lib/libutee/tee_api.c
/optee_os/lib/libutee/tee_api_arith.c
/optee_os/lib/libutee/tee_api_objects.c
/optee_os/lib/libutee/tee_api_operations.c
/optee_os/lib/libutee/tee_api_panic.c
/optee_os/lib/libutee/tee_api_private.h
/optee_os/lib/libutee/tee_api_property.c
/optee_os/lib/libutee/tee_api_se.c
/optee_os/lib/libutee/tee_socket_private.h
/optee_os/lib/libutee/tee_socket_pta.c
/optee_os/lib/libutee/tee_tcpudp_socket.c
/optee_os/lib/libutee/tee_user_mem.c
/optee_os/lib/libutee/tee_user_mem.h
/optee_os/lib/libutee/trace_ext.c
/optee_os/lib/libutee/utee_misc.h
/optee_os/lib/libutils/ext/arch/arm/aeabi_unwind.c
/optee_os/lib/libutils/ext/arch/arm/atomic_a32.S
/optee_os/lib/libutils/ext/arch/arm/atomic_a64.S
/optee_os/lib/libutils/ext/buf_compare_ct.c
/optee_os/lib/libutils/ext/include/asm.S
/optee_os/lib/libutils/ext/include/bitstring.h
/optee_os/lib/libutils/ext/include/compiler.h
/optee_os/lib/libutils/ext/include/printk.h
/optee_os/lib/libutils/ext/include/string_ext.h
/optee_os/lib/libutils/ext/include/trace.h
/optee_os/lib/libutils/ext/include/trace_levels.h
/optee_os/lib/libutils/ext/include/types_ext.h
/optee_os/lib/libutils/ext/include/util.h
/optee_os/lib/libutils/ext/snprintk.c
/optee_os/lib/libutils/ext/strlcat.c
/optee_os/lib/libutils/ext/strlcpy.c
/optee_os/lib/libutils/ext/trace.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_divmod.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_divmod_a32.S
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_ldivmod.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_ldivmod_a32.S
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_shift.c
/optee_os/lib/libutils/isoc/arch/arm/arm32_aeabi_softfloat.c
/optee_os/lib/libutils/isoc/arch/arm/setjmp_a32.S
/optee_os/lib/libutils/isoc/arch/arm/setjmp_a64.S
/optee_os/lib/libutils/isoc/arch/arm/softfloat/arm32_include/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-386-GCC/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-386-GCC/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-386-SSE2-GCC/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-386-SSE2-GCC/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-x86_64-GCC/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Linux-x86_64-GCC/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win32-MinGW/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win32-MinGW/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win32-SSE2-MinGW/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win32-SSE2-MinGW/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win64-MinGW-w64/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/Win64-MinGW-w64/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/template-FAST_INT64/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/template-FAST_INT64/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/template-not-FAST_INT64/Makefile
/optee_os/lib/libutils/isoc/arch/arm/softfloat/build/template-not-FAST_INT64/platform.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/extF80M_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/f128M_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToExtF80UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToF128UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToF32UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_commonNaNToF64UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_extF80MToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_extF80UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_f128MToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_f128UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_f32UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_f64UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNExtF80UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNF128UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNF32UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/s_propagateNaNF64UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/softfloat_raiseFlags.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086-SSE/specialize.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/extF80M_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/f128M_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToExtF80UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToF128UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToF32UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_commonNaNToF64UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_extF80MToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_extF80UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_f128MToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_f128UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_f32UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_f64UIToCommonNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNExtF80UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNF128UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNF32UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/s_propagateNaNF64UI.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/softfloat_raiseFlags.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/8086/specialize.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80M_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/extF80_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_mulAdd.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128M_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_mulAdd.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f128_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_mulAdd.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f32_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_add.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_div.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_eq.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_eq_signaling.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_isSignalingNaN.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_le.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_le_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_lt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_lt_quiet.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_mul.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_mulAdd.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_rem.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_roundToInt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_sqrt.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_sub.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_i32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_i32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_i64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_i64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_ui32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_ui32_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_ui64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/f64_to_ui64_r_minMag.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i32_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/i64_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/internals.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/primitiveTypes.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/primitives.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/softfloat.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/include/softfloat_types.h
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_add128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_add256M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addCarryM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addComplCarryM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addMagsExtF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addMagsF128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addMagsF32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_addMagsF64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_approxRecip32_1.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_approxRecipSqrt32_1.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_compare128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_compare96M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_compareNonnormExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_countLeadingZeros32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_countLeadingZeros64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_countLeadingZeros8.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_eq128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_invalidExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_invalidF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_isNaNF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_le128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_lt128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul128By32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul128MTo256M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul128To256M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul64ByShifted32To128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul64To128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mul64To128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mulAddF128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mulAddF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mulAddF32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_mulAddF64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_negXM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normExtF80SigM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackMToExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackMToF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackToExtF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackToF128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackToF32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normRoundPackToF64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normSubnormalExtF80Sig.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normSubnormalF128Sig.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normSubnormalF128SigM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normSubnormalF32Sig.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_normSubnormalF64Sig.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_remStepMBy32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackMToExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackMToF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackMToI64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackMToUI64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToExtF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToF128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToF32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToF64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToI32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToI64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToUI32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_roundPackToUI64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftLeftM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftNormSigF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam128Extra.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam256M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJam64Extra.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightJamM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shiftRightM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftLeft128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftLeft64To96M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftLeftM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRight128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightExtendM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightJam128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightJam128Extra.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightJam64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightJam64Extra.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightJamM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_shortShiftRightM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_sub128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_sub1XM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_sub256M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_subM.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_subMagsExtF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_subMagsF128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_subMagsF32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_subMagsF64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_tryPropagateNaNExtF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/s_tryPropagateNaNF128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/softfloat_state.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui32_to_f64.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_extF80.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_extF80M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_f128.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_f128M.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_f32.c
/optee_os/lib/libutils/isoc/arch/arm/softfloat/source/ui64_to_f64.c
/optee_os/lib/libutils/isoc/bget_malloc.c
/optee_os/lib/libutils/isoc/include/assert.h
/optee_os/lib/libutils/isoc/include/ctype.h
/optee_os/lib/libutils/isoc/include/inttypes.h
/optee_os/lib/libutils/isoc/include/limits.h
/optee_os/lib/libutils/isoc/include/malloc.h
/optee_os/lib/libutils/isoc/include/memory.h
/optee_os/lib/libutils/isoc/include/setjmp.h
/optee_os/lib/libutils/isoc/include/signal.h
/optee_os/lib/libutils/isoc/include/stdint.h
/optee_os/lib/libutils/isoc/include/stdio.h
/optee_os/lib/libutils/isoc/include/stdlib.h
/optee_os/lib/libutils/isoc/include/string.h
/optee_os/lib/libutils/isoc/include/sys/cdefs.h
/optee_os/lib/libutils/isoc/include/sys/queue.h
/optee_os/lib/libutils/isoc/include/sys/types.h
/optee_os/lib/libutils/isoc/include/time.h
/optee_os/lib/libutils/isoc/include/unistd.h
/optee_os/lib/libutils/isoc/include/wchar.h
/optee_os/lib/libutils/isoc/malloc_lock.c
/optee_os/lib/libutils/isoc/newlib/_ansi.h
/optee_os/lib/libutils/isoc/newlib/abs.c
/optee_os/lib/libutils/isoc/newlib/memchr.c
/optee_os/lib/libutils/isoc/newlib/memcmp.c
/optee_os/lib/libutils/isoc/newlib/memcpy.c
/optee_os/lib/libutils/isoc/newlib/memmove.c
/optee_os/lib/libutils/isoc/newlib/memset.c
/optee_os/lib/libutils/isoc/newlib/strchr.c
/optee_os/lib/libutils/isoc/newlib/strcmp.c
/optee_os/lib/libutils/isoc/newlib/strlen.c
/optee_os/lib/libutils/isoc/newlib/strncmp.c
/optee_os/lib/libutils/isoc/newlib/strnlen.c
/optee_os/lib/libutils/isoc/qsort.c
/optee_os/lib/libutils/isoc/snprintf.c
/optee_os/lib/libutils/isoc/stack_check.c
/optee_os/lib/libutils/isoc/strdup.c
/optee_os/lib/libutils/isoc/strndup.c
/optee_os/scripts/gen_hashed_bin.py
/optee_os/scripts/gen_ld_sects.py
/optee_os/scripts/pem_to_pub_c.py
/optee_os/scripts/symbolize.py
/optee_os/scripts/ta_bin_to_c.py
/optee_os/scripts/tee_bin_parser.py
/optee_os/ta/arch/arm/user_ta_header.c
fb7ef46915-Dec-2017 Jerome Forissier <jerome.forissier@linaro.org>

Reformat copyright/license header in files with an SPDX ID

Some files were committed with an SPDX license identifier before the
rules were defined [1]. Reformat them accordingly.

[1] documentation/

Reformat copyright/license header in files with an SPDX ID

Some files were committed with an SPDX license identifier before the
rules were defined [1]. Reformat them accordingly.

[1] documentation/copyright_and_license_headers.rst

Signed-off-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Joakim Bech <joakim.bech@linaro.org>

show more ...

513b7c9c10-Jan-2018 Jens Wiklander <jens.wiklander@linaro.org>

core: lpae: zero initialize all l1 tables

Fixes: 4cc2823eb25c ("core: user mode translation table")
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Tested-by: Jerome Forissier <jerome.fo

core: lpae: zero initialize all l1 tables

Fixes: 4cc2823eb25c ("core: user mode translation table")
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Tested-by: Jerome Forissier <jerome.forissier@linaro.org> (HiKey)
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>
Tested-by: Jens Wiklander <jens.wiklander@linaro.org> (Hikey)

show more ...

1df3ba0513-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: rename mattr_uflags_to_str()

Renames mattr_uflags_to_str() to mattr_perm_to_str() and report all
permission bits using a 7 bytes long string instead.

This allows observing the permissions of

core: rename mattr_uflags_to_str()

Renames mattr_uflags_to_str() to mattr_perm_to_str() and report all
permission bits using a 7 bytes long string instead.

This allows observing the permissions of the minimal kernel mapping
added to the user space context.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

21a7f5c613-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: make all mapping non-global

Makes all mapping non-global to avoid the otherwise required tlb
invalidation when switching to user mode.

This change makes the fix for CVE-2017-5754 complete.

R

core: make all mapping non-global

Makes all mapping non-global to avoid the otherwise required tlb
invalidation when switching to user mode.

This change makes the fix for CVE-2017-5754 complete.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

5b8a58b413-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: use minimal kernel map in user space

Adds a trampoline in the exception vector to switch to a minimal kernel
map when in user mode. When returning to kernel mode the full kernel
mode map is re

core: use minimal kernel map in user space

Adds a trampoline in the exception vector to switch to a minimal kernel
map when in user mode. When returning to kernel mode the full kernel
mode map is restored.

Arm32 tries to mimic the arm64 exception model somewhat by letting each
exception handler run with disabled asynchronous aborts, irq and fiq.

Form arm32 accesses to the cpus thread_core_local is only done via the
stack pointer in abort mode. Entry of user mode is only done via abort
mode, that means that the abort mode spsr register carries the new cpsr.
Care is taken to have all exceptions disabled while using abort mode.

ASIDs are paired with a user mode ASID with lowest bit sset and a
kernel mode ASID with the lowest bit cleared.

ASID 0 is reserved for kernel mode use when there's no user mode mapping
active.

With this change an active used mode mapping while in kernel mode uses
(asid | 0), and while in user mode (asid | 1). The switch is done via
the trampoline in the vector.

Acked-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

5cee6ca713-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: thread_a32.S: move intr handler macros

Moves the interrupt handler macros closer to the vector.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jero

core: thread_a32.S: move intr handler macros

Moves the interrupt handler macros closer to the vector.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

722b96ee13-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: arm32: exception handlers in one section

Moves all exception handlers into the section of the vector,
.text.thread_vect_table. This makes it possible to later map just the
exception vector and

core: arm32: exception handlers in one section

Moves all exception handlers into the section of the vector,
.text.thread_vect_table. This makes it possible to later map just the
exception vector and the closest associated code while in user mode.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

4cc2823e13-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: user mode translation table

Adds a second translation table to be used while in user mode containing
user mode mapping and a minimal kernel mapping.

Reviewed-by: Etienne Carriere <etienne.car

core: user mode translation table

Adds a second translation table to be used while in user mode containing
user mode mapping and a minimal kernel mapping.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

1a8307fe13-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: mm: add kernel mapping to user map

Adds a minimal kernel mapping needed when user mapping is active.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Andrew Davis <andrew

core: mm: add kernel mapping to user map

Adds a minimal kernel mapping needed when user mapping is active.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

aea6fd2813-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: thread: add thread_get_user_kcode()

Adds thread_get_user_kcode() to report required kernel mapping
(exception vector and some associated code in the same section as the
vector) inside a user m

core: thread: add thread_get_user_kcode()

Adds thread_get_user_kcode() to report required kernel mapping
(exception vector and some associated code in the same section as the
vector) inside a user mapping.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

2c2cb3ab13-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: add mobj_tee_ram

Adds mobj_tee_ram to describe TEE RAM mapping inside a user mapping.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissi

core: add mobj_tee_ram

Adds mobj_tee_ram to describe TEE RAM mapping inside a user mapping.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

9cdfbc7213-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: tlbi_asid() handle kernel mode ASID too

When invalidating an ASID (lowest bit 0), clear the paired ASID (lowest
bit 1)too.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed

core: tlbi_asid() handle kernel mode ASID too

When invalidating an ASID (lowest bit 0), clear the paired ASID (lowest
bit 1)too.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

55705e7613-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: refactor ASID management

Refactors Address Space Identifier management. The field in struct
user_ta_ctx is moved into struct tee_mmu_info and renamed to asid.

Allocation refactored internally

core: refactor ASID management

Refactors Address Space Identifier management. The field in struct
user_ta_ctx is moved into struct tee_mmu_info and renamed to asid.

Allocation refactored internally with asid_alloc() and asid_free()
functions, based on bitstring.h macros.

ASIDs starts at 2, and is always an even number.

ASIDs with the lowest bit set is reserved for as the second ASID when
using ASIDs in pairs.

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Acked-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

33b3d81d13-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: make core_mmu.h asm friendly

Makes core_mmu.h assembly friendly by excluding C code with #ifndef ASM

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier

core: make core_mmu.h asm friendly

Makes core_mmu.h assembly friendly by excluding C code with #ifndef ASM

Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jerome Forissier <jerome.forissier@linaro.org>
Acked-by: Andrew Davis <andrew.davis@linaro.org>
Signed-off-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

ca5e295813-Dec-2017 Jens Wiklander <jens.wiklander@linaro.org>

core: arm32_macros.S: add {read,write}_ttbr0_64bit

Adds the macros read_ttbr0_64bit and write_ttbr0_64bit

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

core: arm32_macros.S: add {read,write}_ttbr0_64bit

Adds the macros read_ttbr0_64bit and write_ttbr0_64bit

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

show more ...

1...<<111112113114115116117118119120>>...162