History log of /optee_os/ (Results 5401 – 5425 of 8578)
Revision Date Author Comments
(<<< Hide modified files)
(Show modified files >>>)
98d863a505-Jul-2019 Jerome Forissier <jerome@forissier.org>

Experimental Clang support

Allows building with Clang with "make COMPILER=clang [other flags...]".
The clang command has to be in the $PATH, as well as the associated
tools (clang-cpp, ld.lld, llvm-

Experimental Clang support

Allows building with Clang with "make COMPILER=clang [other flags...]".
The clang command has to be in the $PATH, as well as the associated
tools (clang-cpp, ld.lld, llvm-ar, llvm-nm, llvm-objcopy and
llvm-readelf).

Tested with Clang built from the master branch of [1] (development
version for 9.0):

mkdir build; cd build
cmake -G Ninja -DCMAKE_BUILD_TYPE=Release \
-DCMAKE_INSTALL_PREFIX=~/llvm-install \
-DLLVM_ENABLE_PROJECTS="clang;lld" \
-DLLVM_TARGETS_TO_BUILD="AArch64;ARM" \
~/llvm-project/llvm
ninja && ninja install

Limitations:

- CFG_CORE_SANITIZE_KADDRESS=y is not supported.
- CFG_WITH_PAGER is supported, but requires that the TEE core be
linked with the GNU linker. The reason is documented in
mk/clang.mk.

Bug:

- ldelf assertion failure in xtest 1019 when CFG_ULIBS_SHARED=y (QEMU)
E/LD: assertion 'maps[map_idx].sz == sz' failed at ldelf/ta_elf.c:1114 in ta_elf_print_mappings()
Prevents ldelf from displaying the TA mappings on abort or panic, but
does not seem to cause any other problem.

Link: [1] https://github.com/llvm/llvm-project/commits/8351c327647
Signed-off-by: Jerome Forissier <jerome@forissier.org>
Tested-by: Jerome Forissier <jerome@forissier.org> (QEMU pager/no pager)
Tested-by: Jerome Forissier <jerome@forissier.org> (QEMUv8, pager/no pager)
Tested-by: Jerome Forissier <jerome@forissier.org> (HiKey960, 32/64, GP)
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

179c8fe826-Mar-2019 Volodymyr Babchuk <vlad.babchuk@gmail.com>

plat/rcar: fix core numbering for M3 flavor

R-car Gen3 SoCs have consistent core numbering across all
variations: CA57 cluster have core numbers 0-3 and CA53 have
numbers 4-7.

M3 flavor have 6 core

plat/rcar: fix core numbering for M3 flavor

R-car Gen3 SoCs have consistent core numbering across all
variations: CA57 cluster have core numbers 0-3 and CA53 have
numbers 4-7.

M3 flavor have 6 cores: two CA57s and four CA53s. Taking
into account consistent numbering, M3 will have the following
core ids: 0, 1, 3, 5, 6, 7. To fix this, we need to set
CFG_CORE_CLUSTER_SHIFT to 1.

This somewhat abuses implementation of get_core_pos_mpidr(),
but it is not expected, that it will change in the future.

Signed-off-by: Volodymyr Babchuk <vlad.babchuk@gmail.com>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

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

build: cfg-depends-one, cfg-depends-all: disable variable with ':= n'

Update cfg-depends-one and cfg-depends-all to use ':= n' to disable a
variable instead of setting it to an empty string. Functio

build: cfg-depends-one, cfg-depends-all: disable variable with ':= n'

Update cfg-depends-one and cfg-depends-all to use ':= n' to disable a
variable instead of setting it to an empty string. Functionally
equivalent but looks better.

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

show more ...

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

build: make cfg-one-enabled return 'n' instead of an empty string

Modify cfg-one-enabled in the same way the parent commit modified
cfg-all-enabled.

Signed-off-by: Jerome Forissier <jerome@forissie

build: make cfg-one-enabled return 'n' instead of an empty string

Modify cfg-one-enabled in the same way the parent commit modified
cfg-all-enabled.

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

show more ...

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

build: make cfg-all-enabled return 'n' instead of an empty string

cfg-all-enabled returns either 'y' or an empty string. Since it is
often used to derive a configuration variable from other ones, it

build: make cfg-all-enabled return 'n' instead of an empty string

cfg-all-enabled returns either 'y' or an empty string. Since it is
often used to derive a configuration variable from other ones, it would
be better to return 'n' instead of an empty string for consistency
(most boolean variables in $O/conf.mk are either 'y' or 'n').

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

show more ...

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

symbolize.py: fix exception when stdin is not a terminal

Commit 6b4fc6752b3c ("symbolize.py: disable terminal local echo") uses
termios functions on stdin unconditionally. Unfortunately, this will
c

symbolize.py: fix exception when stdin is not a terminal

Commit 6b4fc6752b3c ("symbolize.py: disable terminal local echo") uses
termios functions on stdin unconditionally. Unfortunately, this will
cause an exception when stdin is not a terminal, for instance:

$ echo Hello | ./script/symbolize.py
Traceback (most recent call last):
File "./scripts/symbolize.py", line 497, in <module>
main()
File "./scripts/symbolize.py", line 484, in main
old = termios.tcgetattr(fd)
termios.error: (25, 'Inappropriate ioctl for device')

Fix the issue by making sure stdin is a TTY before using the termios
functions.

Fixes: 6b4fc6752b3c ("symbolize.py: disable terminal local echo")
Signed-off-by: Jerome Forissier <jerome@forissier.org>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

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

Revert "hikey: increase core heap size to 192 kB"

This reverts commit 28c75dbebc49 ("hikey: increase core heap size to
192 kB") which increased the core heap size in order to pass the AOSP
VTS. Unfo

Revert "hikey: increase core heap size to 192 kB"

This reverts commit 28c75dbebc49 ("hikey: increase core heap size to
192 kB") which increased the core heap size in order to pass the AOSP
VTS. Unfortunately, this bigger value does not work well when the pager
is enabled: it causes lots of page faults and a massive slowdown (for
instance, 'xtest 1013' on HiKey620 completes in ~ 1.7 s with the
default heap size of 64 kB but takes ~ 53 s with 192 kB).

Therefore, revert to the previous configuration. A bigger value can
always be set on the command line or by other means when building for
AOSP.

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

show more ...

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

core: REE FS TAs: disable CFG_REE_FS_TA_BUFFERED by default

Now that the TA loader is in user space [1], the main reason why we had
introduced CFG_REE_FS_TA_BUFFERED [2] does not exist anymore. Ther

core: REE FS TAs: disable CFG_REE_FS_TA_BUFFERED by default

Now that the TA loader is in user space [1], the main reason why we had
introduced CFG_REE_FS_TA_BUFFERED [2] does not exist anymore. Therefore
we can set it to 'n' by default, thus saving some time and memory.

[1] commit d1911a85142d ("core: load TAs using ldelf")
[2] commit 7db24ad625b9 ("core: REE FS TAs: add option to verify
signature before processing")

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

show more ...

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

symbolize.py: disable terminal local echo

When scripts/symbolize.py is used interactively and the input data is
copied and pasted into the terminal, both the input and output text are
displayed on t

symbolize.py: disable terminal local echo

When scripts/symbolize.py is used interactively and the input data is
copied and pasted into the terminal, both the input and output text are
displayed on the same screen. There is nothing preventing both text
streams from mixing up because it depends on buffering and how Python
reads and flushes its buffers.

Things usually go well with Python 2, but I have observed that Python 3
is more problematic. So the issue needs to be properly addressed. This
patch temporarily disables local echo so that only the processed text is
shown.

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

show more ...

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

core: fix configuration check for CFG_PAGED_USER_TA

The cfg-depends-all function from mk/checkconf.mk has to be enclosed
in a $(eval ...) statement. Fix core/core.mk accordingly.

Signed-off-by: Jer

core: fix configuration check for CFG_PAGED_USER_TA

The cfg-depends-all function from mk/checkconf.mk has to be enclosed
in a $(eval ...) statement. Fix core/core.mk accordingly.

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

show more ...

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

scripts: convert remainging scripts to python3

Convert the remaining scripts to python3. Mostly done with 2to3 and
manual adjustements to the code afterwards.

Signed-off-by: Rouven Czerwinski <r.cz

scripts: convert remainging scripts to python3

Convert the remaining scripts to python3. Mostly done with 2to3 and
manual adjustements to the code afterwards.

Signed-off-by: Rouven Czerwinski <r.czerwinski@pengutronix.de>
Acked-by: Jens Wiklander <jens.wiklander@linaro.org>
Acked-by: Jerome Forissier <jerome@forissier.org>
Tested-by: Jerome Forissier <jerome@forissier.org> (QEMU, QEMUv8)

show more ...

909c706c18-Sep-2019 Etienne Carriere <etienne.carriere@linaro.org>

libutils: relax noreturn label

Replaces attribute label identifier noreturn with __noreturn__ to
prevent conflicts when importing code which defines label noreturn
itself as a macro. This change app

libutils: relax noreturn label

Replaces attribute label identifier noreturn with __noreturn__ to
prevent conflicts when importing code which defines label noreturn
itself as a macro. This change applies suggestion from the GCC
documentation [1], applicable even prio GCC 4.x.x, cited below.

> You may optionally specify attribute names with ‘__’ preceding
> and following the name. This allows you to use them in header
> files without being concerned about a possible macro of the same
> name. For example, you may use the attribute name __noreturn__
> instead of noreturn.

Link: [1] https://gcc.gnu.org/onlinedocs/gcc-8.3.0/gcc/Attribute-Syntax.html#Attribute-Syntax
Signed-off-by: Etienne Carriere <etienne.carriere@linaro.org>
Reviewed-by: Jens Wiklander <jens.wiklander@linaro.org>

show more ...

28c75dbe17-Sep-2019 Victor Chong <victor.chong@linaro.org>

hikey: increase core heap size to 192 kB

To pass VTS in AOSP builds.

Signed-off-by: Victor Chong <victor.chong@linaro.org>
Reviewed-by: Joakim Bech <joakim.bech@linaro.org>

542ae20712-Sep-2019 Cedric Auger <cauger@provenrun.com>

libutee,libdl: remove 0ms timeouts in TA invocations

TEE_OpenTASession(), TEE_InvokeTACommand() calls using 0ms timeout
are replaced with TEE_INFINITE_TIMEOUT to avoid risk of being cancelled.

Sign

libutee,libdl: remove 0ms timeouts in TA invocations

TEE_OpenTASession(), TEE_InvokeTACommand() calls using 0ms timeout
are replaced with TEE_INFINITE_TIMEOUT to avoid risk of being cancelled.

Signed-off-by: Cedric Auger <cauger@provenrun.com>
Reviewed-by: Etienne Carriere <etienne.carriere@linaro.org>

show more ...

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

build: prevent produce-* from being forced built before current submodule

Problem:

$ make -s out/arm-plat-vexpress/core/mm/fobj.o
$ rm out/arm-plat-vexpress/ldelf/ldelf.elf
$ rm out/arm-plat-vex

build: prevent produce-* from being forced built before current submodule

Problem:

$ make -s out/arm-plat-vexpress/core/mm/fobj.o
$ rm out/arm-plat-vexpress/ldelf/ldelf.elf
$ rm out/arm-plat-vexpress/core/mm/fobj.o
$ make out/arm-plat-vexpress/core/mm/fobj.o
CHK out/arm-plat-vexpress/conf.mk
CHK out/arm-plat-vexpress/include/generated/conf.h
LD out/arm-plat-vexpress/ldelf/ldelf.elf
GEN out/arm-plat-vexpress/core/ldelf_hex.c
CC out/arm-plat-vexpress/core/mm/fobj.o

Why would fobj.o depend on ldelf.elf and ldelf_hex.c? Answer is: it
shouldn't. This behavior is caused by FORCE-GENSRC$(sm) depending on
all the produce-<something> targets. In fact, such a dependency is
rarely needed. It makes sense for include files for instance; but
certainly not for C source files which are pulled in the build by other
means.

This patch introduces force-gensrc-<something> to prevent the generated
file $(produce-<something>) from being added to FORCE-GENSRC$(sm)
unless $(force-gensrcs-<something>) is "y". The test case above works
as expected:

$ make -s out/arm-plat-vexpress/core/mm/fobj.o
$ rm out/arm-plat-vexpress/ldelf/ldelf.elf
$ rm out/arm-plat-vexpress/core/mm/fobj.o
$ make out/arm-plat-vexpress/core/mm/fobj.o
CHK out/arm-plat-vexpress/conf.mk
CHK out/arm-plat-vexpress/include/generated/conf.h
CC out/arm-plat-vexpress/core/mm/fobj.o

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

show more ...

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

core: move sockets PTA to core/tee

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

Signed-off-by: Jerome Forissier <jerom

core: move sockets PTA to core/tee

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

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

show more ...

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

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

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

sdp_pta.c is renamed sdp.c since _pta i

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

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

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

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

show more ...

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

core: move test PTAs to core/pta/tests

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

Signed-off

core: move test PTAs to core/pta/tests

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

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

show more ...

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

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

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

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

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

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

show more ...

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

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

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

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

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

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

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

show more ...

172d637b11-Sep-2019 Cedric Auger <cauger@provenrun.com>

libutee: panic on null pointer on object opening

Change TEE_CreatePersistentObject() and TEE_OpenPersistentObject()
to panic when passed an null reference pointer.

According to the TEE Internal Cor

libutee: panic on null pointer on object opening

Change TEE_CreatePersistentObject() and TEE_OpenPersistentObject()
to panic when passed an null reference pointer.

According to the TEE Internal Core API Specification 1.1 and 1.2,
sections 5.7.1 and 5.7.2, passing NULL for object pointer should panic,
and not return an error.

Some harmonization has also been done in these two functions to use
the same conventions as surrounding code.

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

show more ...

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

Squashed commit upgrading to libtomcrypt-1.18.2-develop-20180819

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

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

Squashed commit upgrading to libtomcrypt-1.18.2-develop-20180819

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

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

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

show more ...


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

Revert "compiler.h: introduce GCC version check"

This reverts commit fc78b3ffc59ef03e599ae952b4345f03f466f11c and
updates the comment in <compiler.h>.

It turns out not only GCC 8.x needs the workar

Revert "compiler.h: introduce GCC version check"

This reverts commit fc78b3ffc59ef03e599ae952b4345f03f466f11c and
updates the comment in <compiler.h>.

It turns out not only GCC 8.x needs the workaround. I tried 4.9, 6.2,
8.2, and 8.3 from various sources (Linaro or Ubuntu). If
__SECTION_FLAGS_RODATA is empty, this warning is always present:

CC out/arm-plat-vexpress/core/mm/fobj.o
{standard input}: Assembler messages:
{standard input}:402: Warning: setting incorrect section attributes for .rodata.__unpaged

The generated assembler file contains the "aw" flags:

$ grep '\.section.*\.rodata\.__unpaged' out/arm-plat-vexpress/core/mm/fobj.s
.section .rodata.__unpaged,"aw",%progbits

By reverting the above commit, we have:

$ grep '\.section.*\.rodata\.__unpaged' out/arm-plat-vexpress/core/mm/fobj.s
.section .rodata.__unpaged,"a",%progbits //,"aw",%progbits

...and the assembler does not warn anymore.

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

show more ...

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

ldelf: add __noreturn

The 32-bit variant of e64_relocate() deserves a __noreturn attribute
because it calls utee_return() unconditionally. Fixes a Clang warning.

Signed-off-by: Jerome Forissier <je

ldelf: add __noreturn

The 32-bit variant of e64_relocate() deserves a __noreturn attribute
because it calls utee_return() unconditionally. Fixes a Clang warning.

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

show more ...

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

compiler.h: introduce GCC version check

The macro __SECTION_FLAGS_RODATA introduced by commit fd1187725939 ("core:
force read-only flag on .rodata.* sections") is needed for GCC >= 8, so
it should d

compiler.h: introduce GCC version check

The macro __SECTION_FLAGS_RODATA introduced by commit fd1187725939 ("core:
force read-only flag on .rodata.* sections") is needed for GCC >= 8, so
it should depend on __GCC_VERSION. This prepares for Clang.

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

show more ...

1...<<211212213214215216217218219220>>...344