blob: 01cab3a7e452b7b1720d23e8fb7cd715a82545bc (
plain)
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
|
/*
* Entropy Source Using Intel's rdseed instruction
* (C) 2015 Jack Lloyd, Daniel Neus
*
* Botan is released under the Simplified BSD License (see license.txt)
*/
#include <botan/internal/rdseed.h>
#include <botan/cpuid.h>
#include <botan/build.h>
#if !defined(BOTAN_USE_GCC_INLINE_ASM)
#include <immintrin.h>
#endif
namespace Botan {
BOTAN_FUNC_ISA("rdseed")
size_t Intel_Rdseed::poll(RandomNumberGenerator& rng) {
if(CPUID::has_rdseed())
{
for(size_t p = 0; p != BOTAN_ENTROPY_INTEL_RNG_POLLS; ++p)
{
for(size_t i = 0; i != BOTAN_ENTROPY_RDSEED_RETRIES; ++i)
{
uint32_t r = 0;
#if defined(BOTAN_USE_GCC_INLINE_ASM)
int cf = 0;
// Encoding of rdseed %eax
asm(".byte 0x0F, 0xC7, 0xF8; adcl $0,%1" :
"=a" (r), "=r" (cf) : "0" (r), "1" (cf) : "cc");
#else
int cf = _rdseed32_step(&r);
#endif
if(1 == cf)
{
rng.add_entropy_T(r);
break;
}
}
}
}
return 0;
}
}
|
