5

我在看 HJ Lu 的PATCH: Update x86 rdrand intrinsics。我不知道我是否应该使用_rdrand_u64, _rdrand64_step，或者是否还有其他功能。似乎没有为他们编写测试用例。

似乎也缺少手册页（来自 Ubuntu 14，GCC 4.8.4）：

$ man -k rdrand
rdrand: nothing appropriate.

一个人如何使用RDRAND内在函数来生成一个 32 字节的块？

一个相关的问题是RDRAND 和 RDSEED 内在函数 GCC 和 Intel C++。但它并没有告诉我如何使用它们，或者如何生成一个块。

4

1 回答 1

5

如果您查看<immintrin.h>（我的位于 `/usr/lib/gcc/x86_64-linux-gnu/4.9/include/'，Ubuntu 15.04 64bit），则定义了兼容的（与 MSVC，Intel CC）函数将数据传回GCC 内置

extern __inline int __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_rdrand64_step (unsigned long long *__P)
{
     return __builtin_ia32_rdrand64_step (__P);
}

用于 64 位参数，另外两个用于 16 位和 32 位参数

_rdrand16_step (unsigned short *__P)
_rdrand32_step (unsigned int *__P)

您应该使用这些，以便您的代码与 MSVC、Intel CC 和其他编译器兼容。

_rdrand64_step将填充 64 位参数，通过指针传递，随机位并返回错误代码。32 位和 16 位版本同上

更新

“这些内在函数生成 16/32/64 位宽的随机整数的随机数。生成的随机值被写入给定的内存位置并返回成功状态：如果硬件返回有效的随机值，则为“1”，以及“0” ' 否则。”

https://software.intel.com/en-us/node/523864

更新

根据@vy32 的请求，这对我有用。好吧，我的系统 gt 自原始答案以来已更新，所以现在是 Ubuntu 20.04.1、x64、GCC v9.3、编译标志

gcc -m64 -mrdrnd -O3 a.c

代码

#include <stdio.h>
#include <immintrin.h>

int main() {
    unsigned long long result = 0ULL;

    int rc = _rdrand64_step (&result);

    printf("%i %llu", rc, result);

    return (rc != 1);
}

关于 CF 标志和“忽略这是一个常见的实现错误，在测试中不会出现，但在负载下运行 DRNG 时会出现”，我相信这就是内置的。如果您注释掉 printf 并使用 -S 标志编译为汇编程序，代码将如下所示，

xorl    %eax, %eax
rdrand  %rax
movl    $1, %edx
...    
cmovc   %edx, %eax

这意味着它%eax被归零，%edx被设置为 1，然后cmovc %edx如果 CF 被提升，via 可能被设置为 0。这个值是从函数返回的。

所以我相信内置已经以正确的方式处理进位标志，用户应该_rdrandXX_step(ull*)按照手册中的说明检查输出。

于 2015-07-04T04:37:24.813 回答