Spot of bother compiling an ARMv8 kernel...

[Jon Brawn]

Wotcha!

I’ve got use of a SoftIron OverDrive 1000, and I thought it was about time I updated it to a newer version of 12.0 CURRENT, so I dutifully downloaded the mini memory stick image, installed all the options that the installer offers, rebooted off of the hard drive, and decided that the first thing that one has to do with a new system is build a spangly new kernel.

So:

root at brax:/usr/src # make TARGET=arm64 TARGET_ARCH=aarch64 KERNCONF=GENERIC-NODEBUG kernel

And off it went.

Then, alas, it stopped:

cc -target aarch64-unknown-freebsd12.0 --sysroot=/usr/obj/usr/src/tmp -B/usr/obj/usr/src/tmp/usr/bin -c -O3 -pipe -fno-strict-aliasing -Werror -D_KERNEL -DKLD_MODULE -DHAVE_KERNEL_OPTION_HEADERS -include /usr/obj/usr/src/sys/GENERIC-NODEBUG/opt_global.h -I. -I/usr/src/sys -fno-common -g -fPIC -I/usr/obj/usr/src/sys/GENERIC-NODEBUG -ffixed-x18 -ffreestanding -fwrapv -fstack-protector -gdwarf-2 -Wall -Wredundant-decls -Wnested-externs -Wstrict-prototypes -Wmissing-prototypes -Wpointer-arith -Winline -Wcast-qual -Wundef -Wno-pointer-sign -D__printf__=__freebsd_kprintf__ -Wmissing-include-dirs -fdiagnostics-show-option -Wno-unknown-pragmas -Wno-error-tautological-compare -Wno-error-empty-body -Wno-error-parentheses-equality -Wno-error-unused-function -Wno-error-pointer-sign -Wno-error-shift-negative-value -Wno-error-address-of-packed-member -std=iso9899:1999  -Werror   -march=armv8-a+crypto /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c
In file included from /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:46:
/usr/lib/clang/5.0.0/include/arm_neon.h:31:10: fatal error: 'stdint.h' file not
      found
#include <stdint.h>
         ^~~~~~~~~~
1 error generated.
*** Error code 1

Stop.

What is the freebsd-arm protocol for dealing with this kind of issue? Do I file a bugzilla on it? Or just ask nicely on this list, and someone will say, “Ah, yes, you need to install <mumble> and everything will be alright. Must remember to put that on my to-do list!”? I can work around it easily enough using “The Mark Of Brawn” (what others might call, less charitably, “a bodge”).

Jon.