Spot of bother compiling an ARMv8 kernel...

[Mark Millard]

On 2017-Oct-19, at 9:25 PM, Jon Brawn <jon at brawn.org> wrote:

. . .
> 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
. . .


See also: bugzilla 220125 from back in 2017-Jun-19.

Normally the kernel does not depend on stdint.h but
for this arm NOEN code it does.

make . . . buildworld buildkernel

would work: the buildworld would put the stdint.h in
a place where the buidlkernel would find it.

Unfortunately,

make . . . kernel-toolchain
make . . . buildkernel

would not put the stdint.h in a place that buildkernel
would fine it --and, so, it would error out the same
way.

===
Mark Millard
markmi at dsl-only.net