1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125
126
127
128
129
130
131
132
133
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149
150
151
152
153
154
155
156
157
158
159
160
161
162
163
164
165
166
167
168
169
|
// SPDX-License-Identifier: BSD-2-Clause
/*
* Copyright (c) 2014-2023, Linaro Limited
*/
#include <crypto/crypto.h>
#include <tee_api_types.h>
#include <tee_api_defines.h>
#include <tomcrypt_private.h>
#include <tomcrypt_init.h>
#include "tomcrypt_mp.h"
#include <trace.h>
#if defined(_CFG_CORE_LTC_VFP)
#include <tomcrypt_arm_neon.h>
#include <kernel/thread.h>
#endif
#if defined(_CFG_CORE_LTC_ACIPHER) || defined(_CFG_CORE_LTC_EC25519)
/* Random generator */
static int prng_crypto_start(prng_state *prng __unused)
{
return CRYPT_OK;
}
static int prng_crypto_add_entropy(const unsigned char *in __unused,
unsigned long inlen __unused,
prng_state *prng __unused)
{
/* No entropy is required */
return CRYPT_OK;
}
static int prng_crypto_ready(prng_state *prng __unused)
{
return CRYPT_OK;
}
static unsigned long prng_crypto_read(unsigned char *out, unsigned long outlen,
prng_state *prng __unused)
{
if (crypto_rng_read(out, outlen))
return 0;
return outlen;
}
static int prng_crypto_done(prng_state *prng __unused)
{
return CRYPT_OK;
}
static int prng_crypto_export(unsigned char *out __unused,
unsigned long *outlen __unused,
prng_state *prng __unused)
{
return CRYPT_OK;
}
static int prng_crypto_import(const unsigned char *in __unused,
unsigned long inlen __unused,
prng_state *prng __unused)
{
return CRYPT_OK;
}
static int prng_crypto_test(void)
{
return CRYPT_OK;
}
static const struct ltc_prng_descriptor prng_crypto_desc = {
.name = "prng_crypto",
.export_size = 64,
.start = prng_crypto_start,
.add_entropy = prng_crypto_add_entropy,
.ready = prng_crypto_ready,
.read = prng_crypto_read,
.done = prng_crypto_done,
.pexport = prng_crypto_export,
.pimport = prng_crypto_import,
.test = prng_crypto_test,
};
#endif /*_CFG_CORE_LTC_ACIPHER*/
/*
* tee_ltc_reg_algs(): Registers
* - algorithms
* - hash
* - prng (pseudo random generator)
*/
static void tee_ltc_reg_algs(void)
{
#if defined(_CFG_CORE_LTC_AES) || defined(_CFG_CORE_LTC_AES_DESC)
register_cipher(&aes_desc);
#endif
#if defined(_CFG_CORE_LTC_DES)
register_cipher(&des_desc);
register_cipher(&des3_desc);
#endif
#if defined(_CFG_CORE_LTC_MD5_DESC)
register_hash(&md5_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA1) || defined(_CFG_CORE_LTC_SHA1_DESC)
register_hash(&sha1_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA224) || defined(_CFG_CORE_LTC_SHA224_DESC)
register_hash(&sha224_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA256) || defined(_CFG_CORE_LTC_SHA256_DESC)
register_hash(&sha256_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA384) || defined(_CFG_CORE_LTC_SHA384_DESC)
register_hash(&sha384_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA512) || defined(_CFG_CORE_LTC_SHA512_DESC)
register_hash(&sha512_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA3_224) || defined(_CFG_CORE_LTC_SHA3_224_DESC)
register_hash(&sha3_224_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA3_256) || defined(_CFG_CORE_LTC_SHA3_256_DESC)
register_hash(&sha3_256_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA3_384) || defined(_CFG_CORE_LTC_SHA3_384_DESC)
register_hash(&sha3_384_desc);
#endif
#if defined(_CFG_CORE_LTC_SHA3_512) || defined(_CFG_CORE_LTC_SHA3_512_DESC)
register_hash(&sha3_512_desc);
#endif
#if defined(_CFG_CORE_LTC_ACIPHER) || defined(_CFG_CORE_LTC_EC25519)
register_prng(&prng_crypto_desc);
#endif
}
static void ltc_init(void)
{
#if defined(_CFG_CORE_LTC_ACIPHER)
init_mp_tomcrypt();
#endif
tee_ltc_reg_algs();
}
#if defined(CFG_CRYPTOLIB_NAME_tomcrypt)
TEE_Result crypto_init(void)
{
ltc_init();
return TEE_SUCCESS;
}
#else
void tomcrypt_init(void)
{
ltc_init();
}
#endif
#if defined(CFG_WITH_VFP)
void tomcrypt_arm_neon_enable(struct tomcrypt_arm_neon_state *state)
{
state->state = thread_kernel_enable_vfp();
}
void tomcrypt_arm_neon_disable(struct tomcrypt_arm_neon_state *state)
{
thread_kernel_disable_vfp(state->state);
}
#endif
|
