arch/arm/include/uapi/asm/types.h

   1 /* SPDX-License-Identifier: GPL-2.0 WITH Linux-syscall-note */
   2 #ifndef _UAPI_ASM_TYPES_H
   3 #define _UAPI_ASM_TYPES_H
   4
   5 #include <asm-generic/int-ll64.h>
   6
   7 /*
   8  * The C99 types uintXX_t that are usually defined in 'stdint.h' are not as
   9  * unambiguous on ARM as you would expect. For the types below, there is a
  10  * difference on ARM between GCC built for bare metal ARM, GCC built for glibc
  11  * and the kernel itself, which results in build errors if you try to build with
  12  * -ffreestanding and include 'stdint.h' (such as when you include 'arm_neon.h'
  13  * in order to use NEON intrinsics)
  14  *
  15  * As the typedefs for these types in 'stdint.h' are based on builtin defines
  16  * supplied by GCC, we can tweak these to align with the kernel's idea of those
  17  * types, so 'linux/types.h' and 'stdint.h' can be safely included from the same
  18  * source file (provided that -ffreestanding is used).
  19  *
  20  *                    int32_t         uint32_t               uintptr_t
  21  * bare metal GCC     long            unsigned long          unsigned int
  22  * glibc GCC          int             unsigned int           unsigned int
  23  * kernel             int             unsigned int           unsigned long
  24  */
  25
  26 #ifdef __INT32_TYPE__
  27 #undef __INT32_TYPE__
  28 #define __INT32_TYPE__          int
  29 #endif
  30
  31 #ifdef __UINT32_TYPE__
  32 #undef __UINT32_TYPE__
  33 #define __UINT32_TYPE__ unsigned int
  34 #endif
  35
  36 #ifdef __UINTPTR_TYPE__
  37 #undef __UINTPTR_TYPE__
  38 #define __UINTPTR_TYPE__        unsigned long
  39 #endif
  40
  41 #endif /* _UAPI_ASM_TYPES_H */