Hello, I am currently trying to install the GCC-7 compiler with offloading capabilities for nvptx on the NVIDIA Jetson TX2. Unfortunately without success so far. I used https://gcc.gnu.org/wiki/Offloading and https:// kristerw.blogspot.nl/2017/04/building-gcc-with-support-for-nvidia.html as a main reference. I have adapted the install script provided by the latter reference during the try to resolve the problem (Attached: download.sh and install.sh). I am able to successfully build nvptx-tools, GCC-nvptx and GCC-host compilers without errors. I also tried to use a newer Binutils version (2.30) as suggested here: https://gcc.gnu.org/ml/gcc-help/2017-09/msg00 045.html. But if I try to compile a first openMP example: gcc main.c -O3 -fopenmp -foffload=-lm -v -o prog -lm #include <stdio.h> #include <omp.h> int main() { int nof_dev = 0; int A[1] = {-1}; nof_dev = omp_get_num_devices(); printf("Num. Devices: %d\n",nof_dev); #pragma omp target { A[0] = omp_is_initial_device(); } if (!A[0]) { printf("Able to use offloading!\n"); } return 0; } I get an internal GCC error: mkoffload: internal compiler error: in main, at config/nvptx/mkoffload.c:507. I tried the same procedure also on a bigger machine (x86_64, 256GB RAM and 56 cores) and I was able to run the example. The Jetson TX2 offers on the other hand only 8GB of RAM. Just to be complete: Host compiler: ./aarch64-unknown-linux-gnu-gcc -v Using built-in specs. COLLECT_GCC=./aarch64-unknown-linux-gnu-gcc COLLECT_LTO_WRAPPER=/home/kreilfla/nfs/offload2/install/libexec/gcc/aar ch64-unknown-linux-gnu/7.3.0/lto-wrapper OFFLOAD_TARGET_NAMES=nvptx-none Target: aarch64-unknown-linux-gnu Configured with: ../gcc/configure --build=aarch64-unknown-linux-gnu -- host=aarch64-unknown-linux-gnu --target=aarch64-unknown-linux-gnu -- enable-offload-targets=nvptx-none=/home/kreilfla/nfs/offload2/install --with-cuda-driver-include=/usr/local/cuda/include --with-cuda-driver- lib=/usr/local/cuda/lib64 --disable-bootstrap --disable-multilib -- enable-plugins --enable-languages=c,c++,fortran,lto -- prefix=/home/kreilfla/nfs/offload2/install Thread model: posix gcc version 7.3.0 (GCC) For the accelerator compiler: ./aarch64-unknown-linux-gnu-accel-nvptx-none-gcc -v Using built-in specs. COLLECT_GCC=./aarch64-unknown-linux-gnu-accel-nvptx-none-gcc COLLECT_LTO_WRAPPER=/home/kreilfla/nfs/offload2/install/libexec/gcc/aar ch64-unknown-linux-gnu/7.3.0/accel/nvptx-none/lto-wrapper Target: nvptx-none Configured with: ../gcc/configure --target=nvptx-none --with-build- time-tools=/home/kreilfla/nfs/offload2/install/nvptx-none/bin --enable- as-accelerator-for=aarch64-unknown-linux-gnu --with-newlib --disable- sjlj-exceptions --enable-newlib-io-long-long --enable- languages=c,c++,fortran,lto -- prefix=/home/kreilfla/nfs/offload2/install Thread model: single gcc version 7.3.0 (GCC) I have attached the compile script, preprocessed file and the full compiler output. Unfortunately I do not have a very deep insight into GCC and have not the knowledge to track down where the issue exactly lies. Any pointer or support which helps to solve this problem is highly appreciated because I had no luck in resolving the problem by myself. Thank you very much for your help. Best regards, Flavio Kreiliger
gcc -O3 -fopenmp -foffload=-lm -v -c -o main.o main.c Using built-in specs. COLLECT_GCC=gcc OFFLOAD_TARGET_NAMES=nvptx-none Target: aarch64-unknown-linux-gnu Configured with: ../gcc/configure --build=aarch64-unknown-linux-gnu --host=aarch64-unknown-linux-gnu --target=aarch64-unknown-linux-gnu --enable-offload-targets=nvptx-none=/home/kreilfla/nfs/offload2/install --with-cuda-driver-include=/usr/local/cuda/include --with-cuda-driver-lib=/usr/local/cuda/lib64 --disable-bootstrap --disable-multilib --enable-plugins --enable-languages=c,c++,fortran,lto --prefix=/home/kreilfla/nfs/offload2/install Thread model: posix gcc version 7.3.0 (GCC) COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-c' '-o' 'main.o' '-mlittle-endian' '-mabi=lp64' '-pthread' /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/cc1 -quiet -v -imultiarch aarch64-linux-gnu -D_REENTRANT main.c -quiet -dumpbase main.c -mlittle-endian -mabi=lp64 -auxbase-strip main.o -O3 -version -fopenmp -foffload=-lm -o /tmp/user/1005/ccHFtARC.s GNU C11 (GCC) version 7.3.0 (aarch64-unknown-linux-gnu) compiled by GNU C version 5.4.0 20160609, GMP version 6.1.0, MPFR version 3.1.4, MPC version 1.0.3, isl version isl-0.16.1-GMP GGC heuristics: --param ggc-min-expand=100 --param ggc-min-heapsize=131072 ignoring nonexistent directory "/usr/local/include/aarch64-linux-gnu" ignoring nonexistent directory "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../aarch64-unknown-linux-gnu/include" #include "..." search starts here: #include <...> search starts here: /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include /usr/local/include /home/kreilfla/nfs/offload2/install/include /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include-fixed /usr/include/aarch64-linux-gnu /usr/include End of search list. GNU C11 (GCC) version 7.3.0 (aarch64-unknown-linux-gnu) compiled by GNU C version 5.4.0 20160609, GMP version 6.1.0, MPFR version 3.1.4, MPC version 1.0.3, isl version isl-0.16.1-GMP GGC heuristics: --param ggc-min-expand=100 --param ggc-min-heapsize=131072 Compiler executable checksum: 899a33636bf7764dbff667c428aeed0c COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-c' '-o' 'main.o' '-mlittle-endian' '-mabi=lp64' '-pthread' as -v -EL -mabi=lp64 -o main.o /tmp/user/1005/ccHFtARC.s GNU assembler version 2.30 (aarch64-unknown-linux-gnu) using BFD version (GNU Binutils) 2.30 COMPILER_PATH=/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/ LIBRARY_PATH=/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../lib64/:/lib/aarch64-linux-gnu/:/usr/lib/aarch64-linux-gnu/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../:/lib/:/usr/lib/ COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-c' '-o' 'main.o' '-mlittle-endian' '-mabi=lp64' '-pthread' gcc main.c -O3 -fopenmp -foffload=-lm -v -o prog -lm Using built-in specs. COLLECT_GCC=gcc COLLECT_LTO_WRAPPER=/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/lto-wrapper OFFLOAD_TARGET_NAMES=nvptx-none Target: aarch64-unknown-linux-gnu Configured with: ../gcc/configure --build=aarch64-unknown-linux-gnu --host=aarch64-unknown-linux-gnu --target=aarch64-unknown-linux-gnu --enable-offload-targets=nvptx-none=/home/kreilfla/nfs/offload2/install --with-cuda-driver-include=/usr/local/cuda/include --with-cuda-driver-lib=/usr/local/cuda/lib64 --disable-bootstrap --disable-multilib --enable-plugins --enable-languages=c,c++,fortran,lto --prefix=/home/kreilfla/nfs/offload2/install Thread model: posix gcc version 7.3.0 (GCC) COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-o' 'prog' '-mlittle-endian' '-mabi=lp64' '-pthread' /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/cc1 -quiet -v -imultiarch aarch64-linux-gnu -D_REENTRANT main.c -quiet -dumpbase main.c -mlittle-endian -mabi=lp64 -auxbase main -O3 -version -fopenmp -foffload=-lm -o /tmp/user/1005/cc4ytVdU.s GNU C11 (GCC) version 7.3.0 (aarch64-unknown-linux-gnu) compiled by GNU C version 5.4.0 20160609, GMP version 6.1.0, MPFR version 3.1.4, MPC version 1.0.3, isl version isl-0.16.1-GMP GGC heuristics: --param ggc-min-expand=100 --param ggc-min-heapsize=131072 ignoring nonexistent directory "/usr/local/include/aarch64-linux-gnu" ignoring nonexistent directory "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../aarch64-unknown-linux-gnu/include" #include "..." search starts here: #include <...> search starts here: /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include /usr/local/include /home/kreilfla/nfs/offload2/install/include /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include-fixed /usr/include/aarch64-linux-gnu /usr/include End of search list. GNU C11 (GCC) version 7.3.0 (aarch64-unknown-linux-gnu) compiled by GNU C version 5.4.0 20160609, GMP version 6.1.0, MPFR version 3.1.4, MPC version 1.0.3, isl version isl-0.16.1-GMP GGC heuristics: --param ggc-min-expand=100 --param ggc-min-heapsize=131072 Compiler executable checksum: 899a33636bf7764dbff667c428aeed0c COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-o' 'prog' '-mlittle-endian' '-mabi=lp64' '-pthread' as -v -EL -mabi=lp64 -o /tmp/user/1005/ccM9DXWK.o /tmp/user/1005/cc4ytVdU.s GNU assembler version 2.30 (aarch64-unknown-linux-gnu) using BFD version (GNU Binutils) 2.30 COMPILER_PATH=/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/ LIBRARY_PATH=/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../lib64/:/lib/aarch64-linux-gnu/:/usr/lib/aarch64-linux-gnu/:/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../:/lib/:/usr/lib/ Reading specs from /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../lib64/libgomp.spec COLLECT_GCC_OPTIONS='-O3' '-fopenmp' '-foffload=-lm' '-v' '-o' 'prog' '-mlittle-endian' '-mabi=lp64' '-pthread' /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/collect2 -plugin /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/liblto_plugin.so -plugin-opt=/home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0/lto-wrapper -plugin-opt=-fresolution=/tmp/user/1005/ccmiGrNG.res -plugin-opt=-pass-through=-lgcc -plugin-opt=-pass-through=-lgcc_s -plugin-opt=-pass-through=-lpthread -plugin-opt=-pass-through=-lc -plugin-opt=-pass-through=-lgcc -plugin-opt=-pass-through=-lgcc_s --eh-frame-hdr -dynamic-linker /lib/ld-linux-aarch64.so.1 -X -EL -maarch64linux -o prog /usr/lib/aarch64-linux-gnu/crt1.o /usr/lib/aarch64-linux-gnu/crti.o /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/crtbegin.o /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/crtoffloadbegin.o -L/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0 -L/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../../../lib64 -L/lib/aarch64-linux-gnu -L/usr/lib/aarch64-linux-gnu -L/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/../../.. /tmp/user/1005/ccM9DXWK.o -lm -lgomp -lgcc --as-needed -lgcc_s --no-as-needed -lpthread -lc -lgcc --as-needed -lgcc_s --no-as-needed /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/crtend.o /usr/lib/aarch64-linux-gnu/crtn.o /home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/crtoffloadend.o /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0//accel/nvptx-none/mkoffload @/tmp/user/1005/ccGtNHMe mkoffload: internal compiler error: in main, at config/nvptx/mkoffload.c:507 Please submit a full bug report, with preprocessed source if appropriate. Please include the complete backtrace with any bug report. See <https://gcc.gnu.org/bugs/> for instructions. lto-wrapper: fatal error: /home/kreilfla/nfs/offload2/install/libexec/gcc/aarch64-unknown-linux-gnu/7.3.0//accel/nvptx-none/mkoffload returned 4 exit status compilation terminated. /home/kreilfla/nfs/offload2/install/binutils/bin/ld: error: lto-wrapper failed collect2: error: ld returned 1 exit status Makefile:16: recipe for target 'prog' failed make: *** [prog] Error 1
Attachment:
download.sh
Description: application/shellscript
Attachment:
install.sh
Description: application/shellscript
# 1 "main.c"
# 1 "<built-in>"
# 1 "<command-line>"
# 1 "/usr/include/stdc-predef.h" 1 3 4
# 1 "<command-line>" 2
# 1 "main.c"
# 1 "/usr/include/stdio.h" 1 3 4
# 27 "/usr/include/stdio.h" 3 4
# 1 "/usr/include/features.h" 1 3 4
# 367 "/usr/include/features.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/sys/cdefs.h" 1 3 4
# 410 "/usr/include/aarch64-linux-gnu/sys/cdefs.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/wordsize.h" 1 3 4
# 411 "/usr/include/aarch64-linux-gnu/sys/cdefs.h" 2 3 4
# 368 "/usr/include/features.h" 2 3 4
# 391 "/usr/include/features.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/gnu/stubs.h" 1 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/wordsize.h" 1 3 4
# 6 "/usr/include/aarch64-linux-gnu/gnu/stubs.h" 2 3 4
# 1 "/usr/include/aarch64-linux-gnu/gnu/stubs-lp64.h" 1 3 4
# 9 "/usr/include/aarch64-linux-gnu/gnu/stubs.h" 2 3 4
# 392 "/usr/include/features.h" 2 3 4
# 28 "/usr/include/stdio.h" 2 3 4
# 1 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stddef.h" 1 3 4
# 216 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stddef.h" 3 4
# 216 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stddef.h" 3 4
typedef long unsigned int size_t;
# 34 "/usr/include/stdio.h" 2 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/types.h" 1 3 4
# 27 "/usr/include/aarch64-linux-gnu/bits/types.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/wordsize.h" 1 3 4
# 28 "/usr/include/aarch64-linux-gnu/bits/types.h" 2 3 4
typedef unsigned char __u_char;
typedef unsigned short int __u_short;
typedef unsigned int __u_int;
typedef unsigned long int __u_long;
typedef signed char __int8_t;
typedef unsigned char __uint8_t;
typedef signed short int __int16_t;
typedef unsigned short int __uint16_t;
typedef signed int __int32_t;
typedef unsigned int __uint32_t;
typedef signed long int __int64_t;
typedef unsigned long int __uint64_t;
typedef long int __quad_t;
typedef unsigned long int __u_quad_t;
# 121 "/usr/include/aarch64-linux-gnu/bits/types.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/typesizes.h" 1 3 4
# 122 "/usr/include/aarch64-linux-gnu/bits/types.h" 2 3 4
typedef unsigned long int __dev_t;
typedef unsigned int __uid_t;
typedef unsigned int __gid_t;
typedef unsigned long int __ino_t;
typedef unsigned long int __ino64_t;
typedef unsigned int __mode_t;
typedef unsigned int __nlink_t;
typedef long int __off_t;
typedef long int __off64_t;
typedef int __pid_t;
typedef struct { int __val[2]; } __fsid_t;
typedef long int __clock_t;
typedef unsigned long int __rlim_t;
typedef unsigned long int __rlim64_t;
typedef unsigned int __id_t;
typedef long int __time_t;
typedef unsigned int __useconds_t;
typedef long int __suseconds_t;
typedef int __daddr_t;
typedef int __key_t;
typedef int __clockid_t;
typedef void * __timer_t;
typedef int __blksize_t;
typedef long int __blkcnt_t;
typedef long int __blkcnt64_t;
typedef unsigned long int __fsblkcnt_t;
typedef unsigned long int __fsblkcnt64_t;
typedef unsigned long int __fsfilcnt_t;
typedef unsigned long int __fsfilcnt64_t;
typedef long int __fsword_t;
typedef long int __ssize_t;
typedef long int __syscall_slong_t;
typedef unsigned long int __syscall_ulong_t;
typedef __off64_t __loff_t;
typedef __quad_t *__qaddr_t;
typedef char *__caddr_t;
typedef long int __intptr_t;
typedef unsigned int __socklen_t;
# 36 "/usr/include/stdio.h" 2 3 4
# 44 "/usr/include/stdio.h" 3 4
struct _IO_FILE;
typedef struct _IO_FILE FILE;
# 64 "/usr/include/stdio.h" 3 4
typedef struct _IO_FILE __FILE;
# 74 "/usr/include/stdio.h" 3 4
# 1 "/usr/include/libio.h" 1 3 4
# 31 "/usr/include/libio.h" 3 4
# 1 "/usr/include/_G_config.h" 1 3 4
# 15 "/usr/include/_G_config.h" 3 4
# 1 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stddef.h" 1 3 4
# 16 "/usr/include/_G_config.h" 2 3 4
# 1 "/usr/include/wchar.h" 1 3 4
# 82 "/usr/include/wchar.h" 3 4
typedef struct
{
int __count;
union
{
unsigned int __wch;
char __wchb[4];
} __value;
} __mbstate_t;
# 21 "/usr/include/_G_config.h" 2 3 4
typedef struct
{
__off_t __pos;
__mbstate_t __state;
} _G_fpos_t;
typedef struct
{
__off64_t __pos;
__mbstate_t __state;
} _G_fpos64_t;
# 32 "/usr/include/libio.h" 2 3 4
# 49 "/usr/include/libio.h" 3 4
# 1 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stdarg.h" 1 3 4
# 40 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/stdarg.h" 3 4
typedef __builtin_va_list __gnuc_va_list;
# 50 "/usr/include/libio.h" 2 3 4
# 144 "/usr/include/libio.h" 3 4
struct _IO_jump_t; struct _IO_FILE;
typedef void _IO_lock_t;
struct _IO_marker {
struct _IO_marker *_next;
struct _IO_FILE *_sbuf;
int _pos;
# 173 "/usr/include/libio.h" 3 4
};
enum __codecvt_result
{
__codecvt_ok,
__codecvt_partial,
__codecvt_error,
__codecvt_noconv
};
# 241 "/usr/include/libio.h" 3 4
struct _IO_FILE {
int _flags;
char* _IO_read_ptr;
char* _IO_read_end;
char* _IO_read_base;
char* _IO_write_base;
char* _IO_write_ptr;
char* _IO_write_end;
char* _IO_buf_base;
char* _IO_buf_end;
char *_IO_save_base;
char *_IO_backup_base;
char *_IO_save_end;
struct _IO_marker *_markers;
struct _IO_FILE *_chain;
int _fileno;
int _flags2;
__off_t _old_offset;
unsigned short _cur_column;
signed char _vtable_offset;
char _shortbuf[1];
_IO_lock_t *_lock;
# 289 "/usr/include/libio.h" 3 4
__off64_t _offset;
void *__pad1;
void *__pad2;
void *__pad3;
void *__pad4;
size_t __pad5;
int _mode;
char _unused2[15 * sizeof (int) - 4 * sizeof (void *) - sizeof (size_t)];
};
typedef struct _IO_FILE _IO_FILE;
struct _IO_FILE_plus;
extern struct _IO_FILE_plus _IO_2_1_stdin_;
extern struct _IO_FILE_plus _IO_2_1_stdout_;
extern struct _IO_FILE_plus _IO_2_1_stderr_;
# 333 "/usr/include/libio.h" 3 4
typedef __ssize_t __io_read_fn (void *__cookie, char *__buf, size_t __nbytes);
typedef __ssize_t __io_write_fn (void *__cookie, const char *__buf,
size_t __n);
typedef int __io_seek_fn (void *__cookie, __off64_t *__pos, int __w);
typedef int __io_close_fn (void *__cookie);
# 385 "/usr/include/libio.h" 3 4
extern int __underflow (_IO_FILE *);
extern int __uflow (_IO_FILE *);
extern int __overflow (_IO_FILE *, int);
# 429 "/usr/include/libio.h" 3 4
extern int _IO_getc (_IO_FILE *__fp);
extern int _IO_putc (int __c, _IO_FILE *__fp);
extern int _IO_feof (_IO_FILE *__fp) __attribute__ ((__nothrow__ , __leaf__));
extern int _IO_ferror (_IO_FILE *__fp) __attribute__ ((__nothrow__ , __leaf__));
extern int _IO_peekc_locked (_IO_FILE *__fp);
extern void _IO_flockfile (_IO_FILE *) __attribute__ ((__nothrow__ , __leaf__));
extern void _IO_funlockfile (_IO_FILE *) __attribute__ ((__nothrow__ , __leaf__));
extern int _IO_ftrylockfile (_IO_FILE *) __attribute__ ((__nothrow__ , __leaf__));
# 459 "/usr/include/libio.h" 3 4
extern int _IO_vfscanf (_IO_FILE * __restrict, const char * __restrict,
__gnuc_va_list, int *__restrict);
extern int _IO_vfprintf (_IO_FILE *__restrict, const char *__restrict,
__gnuc_va_list);
extern __ssize_t _IO_padn (_IO_FILE *, int, __ssize_t);
extern size_t _IO_sgetn (_IO_FILE *, void *, size_t);
extern __off64_t _IO_seekoff (_IO_FILE *, __off64_t, int, int);
extern __off64_t _IO_seekpos (_IO_FILE *, __off64_t, int);
extern void _IO_free_backup_area (_IO_FILE *) __attribute__ ((__nothrow__ , __leaf__));
# 75 "/usr/include/stdio.h" 2 3 4
typedef __gnuc_va_list va_list;
# 90 "/usr/include/stdio.h" 3 4
typedef __off_t off_t;
# 102 "/usr/include/stdio.h" 3 4
typedef __ssize_t ssize_t;
typedef _G_fpos_t fpos_t;
# 164 "/usr/include/stdio.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/stdio_lim.h" 1 3 4
# 165 "/usr/include/stdio.h" 2 3 4
extern struct _IO_FILE *stdin;
extern struct _IO_FILE *stdout;
extern struct _IO_FILE *stderr;
extern int remove (const char *__filename) __attribute__ ((__nothrow__ , __leaf__));
extern int rename (const char *__old, const char *__new) __attribute__ ((__nothrow__ , __leaf__));
extern int renameat (int __oldfd, const char *__old, int __newfd,
const char *__new) __attribute__ ((__nothrow__ , __leaf__));
extern FILE *tmpfile (void) ;
# 209 "/usr/include/stdio.h" 3 4
extern char *tmpnam (char *__s) __attribute__ ((__nothrow__ , __leaf__)) ;
extern char *tmpnam_r (char *__s) __attribute__ ((__nothrow__ , __leaf__)) ;
# 227 "/usr/include/stdio.h" 3 4
extern char *tempnam (const char *__dir, const char *__pfx)
__attribute__ ((__nothrow__ , __leaf__)) __attribute__ ((__malloc__)) ;
extern int fclose (FILE *__stream);
extern int fflush (FILE *__stream);
# 252 "/usr/include/stdio.h" 3 4
extern int fflush_unlocked (FILE *__stream);
# 266 "/usr/include/stdio.h" 3 4
extern FILE *fopen (const char *__restrict __filename,
const char *__restrict __modes) ;
extern FILE *freopen (const char *__restrict __filename,
const char *__restrict __modes,
FILE *__restrict __stream) ;
# 295 "/usr/include/stdio.h" 3 4
# 306 "/usr/include/stdio.h" 3 4
extern FILE *fdopen (int __fd, const char *__modes) __attribute__ ((__nothrow__ , __leaf__)) ;
# 319 "/usr/include/stdio.h" 3 4
extern FILE *fmemopen (void *__s, size_t __len, const char *__modes)
__attribute__ ((__nothrow__ , __leaf__)) ;
extern FILE *open_memstream (char **__bufloc, size_t *__sizeloc) __attribute__ ((__nothrow__ , __leaf__)) ;
extern void setbuf (FILE *__restrict __stream, char *__restrict __buf) __attribute__ ((__nothrow__ , __leaf__));
extern int setvbuf (FILE *__restrict __stream, char *__restrict __buf,
int __modes, size_t __n) __attribute__ ((__nothrow__ , __leaf__));
extern void setbuffer (FILE *__restrict __stream, char *__restrict __buf,
size_t __size) __attribute__ ((__nothrow__ , __leaf__));
extern void setlinebuf (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__));
extern int fprintf (FILE *__restrict __stream,
const char *__restrict __format, ...);
extern int printf (const char *__restrict __format, ...);
extern int sprintf (char *__restrict __s,
const char *__restrict __format, ...) __attribute__ ((__nothrow__));
extern int vfprintf (FILE *__restrict __s, const char *__restrict __format,
__gnuc_va_list __arg);
extern int vprintf (const char *__restrict __format, __gnuc_va_list __arg);
extern int vsprintf (char *__restrict __s, const char *__restrict __format,
__gnuc_va_list __arg) __attribute__ ((__nothrow__));
extern int snprintf (char *__restrict __s, size_t __maxlen,
const char *__restrict __format, ...)
__attribute__ ((__nothrow__)) __attribute__ ((__format__ (__printf__, 3, 4)));
extern int vsnprintf (char *__restrict __s, size_t __maxlen,
const char *__restrict __format, __gnuc_va_list __arg)
__attribute__ ((__nothrow__)) __attribute__ ((__format__ (__printf__, 3, 0)));
# 412 "/usr/include/stdio.h" 3 4
extern int vdprintf (int __fd, const char *__restrict __fmt,
__gnuc_va_list __arg)
__attribute__ ((__format__ (__printf__, 2, 0)));
extern int dprintf (int __fd, const char *__restrict __fmt, ...)
__attribute__ ((__format__ (__printf__, 2, 3)));
extern int fscanf (FILE *__restrict __stream,
const char *__restrict __format, ...) ;
extern int scanf (const char *__restrict __format, ...) ;
extern int sscanf (const char *__restrict __s,
const char *__restrict __format, ...) __attribute__ ((__nothrow__ , __leaf__));
# 443 "/usr/include/stdio.h" 3 4
extern int fscanf (FILE *__restrict __stream, const char *__restrict __format, ...) __asm__ ("" "__isoc99_fscanf")
;
extern int scanf (const char *__restrict __format, ...) __asm__ ("" "__isoc99_scanf")
;
extern int sscanf (const char *__restrict __s, const char *__restrict __format, ...) __asm__ ("" "__isoc99_sscanf") __attribute__ ((__nothrow__ , __leaf__))
;
# 463 "/usr/include/stdio.h" 3 4
extern int vfscanf (FILE *__restrict __s, const char *__restrict __format,
__gnuc_va_list __arg)
__attribute__ ((__format__ (__scanf__, 2, 0))) ;
extern int vscanf (const char *__restrict __format, __gnuc_va_list __arg)
__attribute__ ((__format__ (__scanf__, 1, 0))) ;
extern int vsscanf (const char *__restrict __s,
const char *__restrict __format, __gnuc_va_list __arg)
__attribute__ ((__nothrow__ , __leaf__)) __attribute__ ((__format__ (__scanf__, 2, 0)));
# 494 "/usr/include/stdio.h" 3 4
extern int vfscanf (FILE *__restrict __s, const char *__restrict __format, __gnuc_va_list __arg) __asm__ ("" "__isoc99_vfscanf")
__attribute__ ((__format__ (__scanf__, 2, 0))) ;
extern int vscanf (const char *__restrict __format, __gnuc_va_list __arg) __asm__ ("" "__isoc99_vscanf")
__attribute__ ((__format__ (__scanf__, 1, 0))) ;
extern int vsscanf (const char *__restrict __s, const char *__restrict __format, __gnuc_va_list __arg) __asm__ ("" "__isoc99_vsscanf") __attribute__ ((__nothrow__ , __leaf__))
__attribute__ ((__format__ (__scanf__, 2, 0)));
# 522 "/usr/include/stdio.h" 3 4
extern int fgetc (FILE *__stream);
extern int getc (FILE *__stream);
extern int getchar (void);
# 550 "/usr/include/stdio.h" 3 4
extern int getc_unlocked (FILE *__stream);
extern int getchar_unlocked (void);
# 561 "/usr/include/stdio.h" 3 4
extern int fgetc_unlocked (FILE *__stream);
extern int fputc (int __c, FILE *__stream);
extern int putc (int __c, FILE *__stream);
extern int putchar (int __c);
# 594 "/usr/include/stdio.h" 3 4
extern int fputc_unlocked (int __c, FILE *__stream);
extern int putc_unlocked (int __c, FILE *__stream);
extern int putchar_unlocked (int __c);
extern int getw (FILE *__stream);
extern int putw (int __w, FILE *__stream);
extern char *fgets (char *__restrict __s, int __n, FILE *__restrict __stream)
;
# 640 "/usr/include/stdio.h" 3 4
# 665 "/usr/include/stdio.h" 3 4
extern __ssize_t __getdelim (char **__restrict __lineptr,
size_t *__restrict __n, int __delimiter,
FILE *__restrict __stream) ;
extern __ssize_t getdelim (char **__restrict __lineptr,
size_t *__restrict __n, int __delimiter,
FILE *__restrict __stream) ;
extern __ssize_t getline (char **__restrict __lineptr,
size_t *__restrict __n,
FILE *__restrict __stream) ;
extern int fputs (const char *__restrict __s, FILE *__restrict __stream);
extern int puts (const char *__s);
extern int ungetc (int __c, FILE *__stream);
extern size_t fread (void *__restrict __ptr, size_t __size,
size_t __n, FILE *__restrict __stream) ;
extern size_t fwrite (const void *__restrict __ptr, size_t __size,
size_t __n, FILE *__restrict __s);
# 737 "/usr/include/stdio.h" 3 4
extern size_t fread_unlocked (void *__restrict __ptr, size_t __size,
size_t __n, FILE *__restrict __stream) ;
extern size_t fwrite_unlocked (const void *__restrict __ptr, size_t __size,
size_t __n, FILE *__restrict __stream);
extern int fseek (FILE *__stream, long int __off, int __whence);
extern long int ftell (FILE *__stream) ;
extern void rewind (FILE *__stream);
# 773 "/usr/include/stdio.h" 3 4
extern int fseeko (FILE *__stream, __off_t __off, int __whence);
extern __off_t ftello (FILE *__stream) ;
# 792 "/usr/include/stdio.h" 3 4
extern int fgetpos (FILE *__restrict __stream, fpos_t *__restrict __pos);
extern int fsetpos (FILE *__stream, const fpos_t *__pos);
# 815 "/usr/include/stdio.h" 3 4
# 824 "/usr/include/stdio.h" 3 4
extern void clearerr (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__));
extern int feof (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern int ferror (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern void clearerr_unlocked (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__));
extern int feof_unlocked (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern int ferror_unlocked (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern void perror (const char *__s);
# 1 "/usr/include/aarch64-linux-gnu/bits/sys_errlist.h" 1 3 4
# 26 "/usr/include/aarch64-linux-gnu/bits/sys_errlist.h" 3 4
extern int sys_nerr;
extern const char *const sys_errlist[];
# 854 "/usr/include/stdio.h" 2 3 4
extern int fileno (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern int fileno_unlocked (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
# 872 "/usr/include/stdio.h" 3 4
extern FILE *popen (const char *__command, const char *__modes) ;
extern int pclose (FILE *__stream);
extern char *ctermid (char *__s) __attribute__ ((__nothrow__ , __leaf__));
# 912 "/usr/include/stdio.h" 3 4
extern void flockfile (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__));
extern int ftrylockfile (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__)) ;
extern void funlockfile (FILE *__stream) __attribute__ ((__nothrow__ , __leaf__));
# 933 "/usr/include/stdio.h" 3 4
# 1 "/usr/include/aarch64-linux-gnu/bits/stdio.h" 1 3 4
# 35 "/usr/include/aarch64-linux-gnu/bits/stdio.h" 3 4
extern __inline __attribute__ ((__gnu_inline__)) int
vprintf (const char *__restrict __fmt, __gnuc_va_list __arg)
{
return vfprintf (stdout, __fmt, __arg);
}
extern __inline __attribute__ ((__gnu_inline__)) int
getchar (void)
{
return _IO_getc (stdin);
}
extern __inline __attribute__ ((__gnu_inline__)) int
fgetc_unlocked (FILE *__fp)
{
return (__builtin_expect (((__fp)->_IO_read_ptr >= (__fp)->_IO_read_end), 0) ? __uflow (__fp) : *(unsigned char *) (__fp)->_IO_read_ptr++);
}
extern __inline __attribute__ ((__gnu_inline__)) int
getc_unlocked (FILE *__fp)
{
return (__builtin_expect (((__fp)->_IO_read_ptr >= (__fp)->_IO_read_end), 0) ? __uflow (__fp) : *(unsigned char *) (__fp)->_IO_read_ptr++);
}
extern __inline __attribute__ ((__gnu_inline__)) int
getchar_unlocked (void)
{
return (__builtin_expect (((stdin)->_IO_read_ptr >= (stdin)->_IO_read_end), 0) ? __uflow (stdin) : *(unsigned char *) (stdin)->_IO_read_ptr++);
}
extern __inline __attribute__ ((__gnu_inline__)) int
putchar (int __c)
{
return _IO_putc (__c, stdout);
}
extern __inline __attribute__ ((__gnu_inline__)) int
fputc_unlocked (int __c, FILE *__stream)
{
return (__builtin_expect (((__stream)->_IO_write_ptr >= (__stream)->_IO_write_end), 0) ? __overflow (__stream, (unsigned char) (__c)) : (unsigned char) (*(__stream)->_IO_write_ptr++ = (__c)));
}
extern __inline __attribute__ ((__gnu_inline__)) int
putc_unlocked (int __c, FILE *__stream)
{
return (__builtin_expect (((__stream)->_IO_write_ptr >= (__stream)->_IO_write_end), 0) ? __overflow (__stream, (unsigned char) (__c)) : (unsigned char) (*(__stream)->_IO_write_ptr++ = (__c)));
}
extern __inline __attribute__ ((__gnu_inline__)) int
putchar_unlocked (int __c)
{
return (__builtin_expect (((stdout)->_IO_write_ptr >= (stdout)->_IO_write_end), 0) ? __overflow (stdout, (unsigned char) (__c)) : (unsigned char) (*(stdout)->_IO_write_ptr++ = (__c)));
}
# 124 "/usr/include/aarch64-linux-gnu/bits/stdio.h" 3 4
extern __inline __attribute__ ((__gnu_inline__)) int
__attribute__ ((__nothrow__ , __leaf__)) feof_unlocked (FILE *__stream)
{
return (((__stream)->_flags & 0x10) != 0);
}
extern __inline __attribute__ ((__gnu_inline__)) int
__attribute__ ((__nothrow__ , __leaf__)) ferror_unlocked (FILE *__stream)
{
return (((__stream)->_flags & 0x20) != 0);
}
# 934 "/usr/include/stdio.h" 2 3 4
# 942 "/usr/include/stdio.h" 3 4
# 2 "main.c" 2
# 1 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/omp.h" 1 3 4
# 35 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/omp.h" 3 4
typedef struct
{
unsigned char _x[4]
__attribute__((__aligned__(4)));
} omp_lock_t;
typedef struct
{
unsigned char _x[16]
__attribute__((__aligned__(8)));
} omp_nest_lock_t;
typedef enum omp_sched_t
{
omp_sched_static = 1,
omp_sched_dynamic = 2,
omp_sched_guided = 3,
omp_sched_auto = 4
} omp_sched_t;
typedef enum omp_proc_bind_t
{
omp_proc_bind_false = 0,
omp_proc_bind_true = 1,
omp_proc_bind_master = 2,
omp_proc_bind_close = 3,
omp_proc_bind_spread = 4
} omp_proc_bind_t;
typedef enum omp_lock_hint_t
{
omp_lock_hint_none = 0,
omp_lock_hint_uncontended = 1,
omp_lock_hint_contended = 2,
omp_lock_hint_nonspeculative = 4,
omp_lock_hint_speculative = 8,
} omp_lock_hint_t;
# 81 "/home/kreilfla/nfs/offload2/install/lib/gcc/aarch64-unknown-linux-gnu/7.3.0/include/omp.h" 3 4
extern void omp_set_num_threads (int) __attribute__((__nothrow__));
extern int omp_get_num_threads (void) __attribute__((__nothrow__));
extern int omp_get_max_threads (void) __attribute__((__nothrow__));
extern int omp_get_thread_num (void) __attribute__((__nothrow__));
extern int omp_get_num_procs (void) __attribute__((__nothrow__));
extern int omp_in_parallel (void) __attribute__((__nothrow__));
extern void omp_set_dynamic (int) __attribute__((__nothrow__));
extern int omp_get_dynamic (void) __attribute__((__nothrow__));
extern void omp_set_nested (int) __attribute__((__nothrow__));
extern int omp_get_nested (void) __attribute__((__nothrow__));
extern void omp_init_lock (omp_lock_t *) __attribute__((__nothrow__));
extern void omp_init_lock_with_hint (omp_lock_t *, omp_lock_hint_t)
__attribute__((__nothrow__));
extern void omp_destroy_lock (omp_lock_t *) __attribute__((__nothrow__));
extern void omp_set_lock (omp_lock_t *) __attribute__((__nothrow__));
extern void omp_unset_lock (omp_lock_t *) __attribute__((__nothrow__));
extern int omp_test_lock (omp_lock_t *) __attribute__((__nothrow__));
extern void omp_init_nest_lock (omp_nest_lock_t *) __attribute__((__nothrow__));
extern void omp_init_nest_lock_with_hint (omp_lock_t *, omp_lock_hint_t)
__attribute__((__nothrow__));
extern void omp_destroy_nest_lock (omp_nest_lock_t *) __attribute__((__nothrow__));
extern void omp_set_nest_lock (omp_nest_lock_t *) __attribute__((__nothrow__));
extern void omp_unset_nest_lock (omp_nest_lock_t *) __attribute__((__nothrow__));
extern int omp_test_nest_lock (omp_nest_lock_t *) __attribute__((__nothrow__));
extern double omp_get_wtime (void) __attribute__((__nothrow__));
extern double omp_get_wtick (void) __attribute__((__nothrow__));
extern void omp_set_schedule (omp_sched_t, int) __attribute__((__nothrow__));
extern void omp_get_schedule (omp_sched_t *, int *) __attribute__((__nothrow__));
extern int omp_get_thread_limit (void) __attribute__((__nothrow__));
extern void omp_set_max_active_levels (int) __attribute__((__nothrow__));
extern int omp_get_max_active_levels (void) __attribute__((__nothrow__));
extern int omp_get_level (void) __attribute__((__nothrow__));
extern int omp_get_ancestor_thread_num (int) __attribute__((__nothrow__));
extern int omp_get_team_size (int) __attribute__((__nothrow__));
extern int omp_get_active_level (void) __attribute__((__nothrow__));
extern int omp_in_final (void) __attribute__((__nothrow__));
extern int omp_get_cancellation (void) __attribute__((__nothrow__));
extern omp_proc_bind_t omp_get_proc_bind (void) __attribute__((__nothrow__));
extern int omp_get_num_places (void) __attribute__((__nothrow__));
extern int omp_get_place_num_procs (int) __attribute__((__nothrow__));
extern void omp_get_place_proc_ids (int, int *) __attribute__((__nothrow__));
extern int omp_get_place_num (void) __attribute__((__nothrow__));
extern int omp_get_partition_num_places (void) __attribute__((__nothrow__));
extern void omp_get_partition_place_nums (int *) __attribute__((__nothrow__));
extern void omp_set_default_device (int) __attribute__((__nothrow__));
extern int omp_get_default_device (void) __attribute__((__nothrow__));
extern int omp_get_num_devices (void) __attribute__((__nothrow__));
extern int omp_get_num_teams (void) __attribute__((__nothrow__));
extern int omp_get_team_num (void) __attribute__((__nothrow__));
extern int omp_is_initial_device (void) __attribute__((__nothrow__));
extern int omp_get_initial_device (void) __attribute__((__nothrow__));
extern int omp_get_max_task_priority (void) __attribute__((__nothrow__));
extern void *omp_target_alloc (long unsigned int, int) __attribute__((__nothrow__));
extern void omp_target_free (void *, int) __attribute__((__nothrow__));
extern int omp_target_is_present (void *, int) __attribute__((__nothrow__));
extern int omp_target_memcpy (void *, void *, long unsigned int, long unsigned int,
long unsigned int, int, int) __attribute__((__nothrow__));
extern int omp_target_memcpy_rect (void *, void *, long unsigned int, int,
const long unsigned int *,
const long unsigned int *,
const long unsigned int *,
const long unsigned int *,
const long unsigned int *, int, int)
__attribute__((__nothrow__));
extern int omp_target_associate_ptr (void *, void *, long unsigned int,
long unsigned int, int) __attribute__((__nothrow__));
extern int omp_target_disassociate_ptr (void *, int) __attribute__((__nothrow__));
# 3 "main.c" 2
# 4 "main.c"
int main() {
int nof_dev = 0;
int A[1] = {-1};
nof_dev = omp_get_num_devices();
printf("Num. Devices: %d\n",nof_dev);
# 11 "main.c"
#pragma omp target
# 11 "main.c"
{
A[0] = omp_is_initial_device();
}
if (!A[0]) {
printf("Able to use offloading!\n");
}
return 0;
}
