1/*===---- rdseedintrin.h - RDSEED intrinsics -------------------------------===
  2 *
  3 * Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
  4 * See https://llvm.org/LICENSE.txt for license information.
  5 * SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
  6 *
  7 *===-----------------------------------------------------------------------===
  8 */
  9
 10#ifndef __IMMINTRIN_H
 11#error "Never use <rdseedintrin.h> directly; include <immintrin.h> instead."
 12#endif
 13
 14#ifndef __RDSEEDINTRIN_H
 15#define __RDSEEDINTRIN_H
 16
 17/* Define the default attributes for the functions in this file. */
 18#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("rdseed")))
 19
 20/// Stores a hardware-generated 16-bit random value in the memory at \a __p.
 21///
 22///    The random number generator complies with NIST SP800-90B and SP800-90C.
 23///
 24/// \code{.operation}
 25/// IF HW_NRND_GEN.ready == 1
 26///   Store16(__p, HW_NRND_GEN.data)
 27///   result := 1
 28/// ELSE
 29///   Store16(__p, 0)
 30///   result := 0
 31/// END
 32/// \endcode
 33///
 34/// \headerfile <immintrin.h>
 35///
 36/// This intrinsic corresponds to the \c RDSEED instruction.
 37///
 38/// \param __p
 39///    Pointer to memory for storing the 16-bit random number.
 40/// \returns 1 if a random number was generated, 0 if not.
 41static __inline__ int __DEFAULT_FN_ATTRS
 42_rdseed16_step(unsigned short *__p)
 43{
 44  return (int) __builtin_ia32_rdseed16_step(__p);
 45}
 46
 47/// Stores a hardware-generated 32-bit random value in the memory at \a __p.
 48///
 49///    The random number generator complies with NIST SP800-90B and SP800-90C.
 50///
 51/// \code{.operation}
 52/// IF HW_NRND_GEN.ready == 1
 53///   Store32(__p, HW_NRND_GEN.data)
 54///   result := 1
 55/// ELSE
 56///   Store32(__p, 0)
 57///   result := 0
 58/// END
 59/// \endcode
 60///
 61/// \headerfile <immintrin.h>
 62///
 63/// This intrinsic corresponds to the \c RDSEED instruction.
 64///
 65/// \param __p
 66///    Pointer to memory for storing the 32-bit random number.
 67/// \returns 1 if a random number was generated, 0 if not.
 68static __inline__ int __DEFAULT_FN_ATTRS
 69_rdseed32_step(unsigned int *__p)
 70{
 71  return (int) __builtin_ia32_rdseed32_step(__p);
 72}
 73
 74#ifdef __x86_64__
 75/// Stores a hardware-generated 64-bit random value in the memory at \a __p.
 76///
 77///    The random number generator complies with NIST SP800-90B and SP800-90C.
 78///
 79/// \code{.operation}
 80/// IF HW_NRND_GEN.ready == 1
 81///   Store64(__p, HW_NRND_GEN.data)
 82///   result := 1
 83/// ELSE
 84///   Store64(__p, 0)
 85///   result := 0
 86/// END
 87/// \endcode
 88///
 89/// \headerfile <immintrin.h>
 90///
 91/// This intrinsic corresponds to the \c RDSEED instruction.
 92///
 93/// \param __p
 94///    Pointer to memory for storing the 64-bit random number.
 95/// \returns 1 if a random number was generated, 0 if not.
 96static __inline__ int __DEFAULT_FN_ATTRS
 97_rdseed64_step(unsigned long long *__p)
 98{
 99  return (int) __builtin_ia32_rdseed64_step(__p);
100}
101#endif
102
103#undef __DEFAULT_FN_ATTRS
104
105#endif /* __RDSEEDINTRIN_H */