kernel-toolchain did not create stdint.h for amd64 -> arm64.aarch64 head -r323246 cross build so buildkernel failed

[Mark Millard]

The failure was:

--- armv8_crypto_wrap.o ---
In file included from /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:46:
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/lib/clang/5.0.0/include/arm_neon.h:31:10: fatal error: 'stdint.h' file not found
#include <stdint.h>
         ^~~~~~~~~~

Context:

# uname -apKU
FreeBSD FreeBSDx64OPC 12.0-CURRENT FreeBSD 12.0-CURRENT  r323246M  amd64 amd64 1200043 1200043

# svnlite info /usr/src/ | grep "Re[plv]"
Relative URL: ^/head
Repository Root: svn://svn.freebsd.org/base
Repository UUID: ccf9f872-aa2e-dd11-9fc8-001c23d0bc1f
Revision: 323246
Last Changed Rev: 323246

Note: The problem is repeatable.


[Note: /usr/obj/cortexA53dbg_clang/arm64.aarch64/ was empty at the start
of the below.]

The failure was after:

# ~/sys_build_scripts.amd64-host/make_cortexA53_debug_clang_bootstrap-amd64-host.sh -j14 kernel-toolchain
Script started, output file is /root/sys_typescripts/typescript_make_cortexA53_debug_clang_bootstrap-amd64-host-2017-09-08:13:46:59
--- kernel-toolchain ---
make[1]: "/usr/src/Makefile.inc1" line 688: META_MODE: Rebuilding host tools due to ABI breakage in __FreeBSD_version 1200031.
--- _worldtmp ---

--------------------------------------------------------------
>>> Rebuilding the temporary build tree
--------------------------------------------------------------
rm -rf /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr/include
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/lib
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/lib/casper
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/bin
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr
. . .

from which there was no stdint.h :

# find /usr/obj/cortexA53dbg_clang/ -name stdint.h -print
# 


In more detail:


# ~/sys_build_scripts.amd64-host/make_cortexA53_debug_clang_bootstrap-amd64-host.sh -j14 kernel-toolchain
Script started, output file is /root/sys_typescripts/typescript_make_cortexA53_debug_clang_bootstrap-amd64-host-2017-09-08:13:46:59
--- kernel-toolchain ---
make[1]: "/usr/src/Makefile.inc1" line 688: META_MODE: Rebuilding host tools due to ABI breakage in __FreeBSD_version 1200031.
--- _worldtmp ---

--------------------------------------------------------------
>>> Rebuilding the temporary build tree
--------------------------------------------------------------
rm -rf /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr/include
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/lib
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/lib/casper
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/bin
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr
. . .

Building /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/host-osreldate.h

Script done, output file is /root/sys_typescripts/typescript_make_cortexA53_debug_clang_bootstrap-amd64-host-2017-09-08:13:46:59

# ~/sys_build_scripts.amd64-host/make_cortexA53_debug_clang_bootstrap-amd64-host.sh -j14 buildkernel
Script started, output file is /root/sys_typescripts/typescript_make_cortexA53_debug_clang_bootstrap-amd64-host-2017-09-08:19:14:18
--- buildkernel ---
--- buildkernel ---

--------------------------------------------------------------
>>> Kernel build for GENERIC-DBG started on Fri Sep  8 19:14:18 PDT 2017
--------------------------------------------------------------
===> GENERIC-DBG
mkdir -p /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys
--------------------------------------------------------------
>>> stage 1: configuring the kernel
--------------------------------------------------------------
. . .

--- armv8_crypto_wrap.o ---
In file included from /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:46:
/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/lib/clang/5.0.0/include/arm_neon.h:31:10: fatal error: 'stdint.h' file not found
#include <stdint.h>
         ^~~~~~~~~~


--- all_subdir_armv8crypto ---
1 error generated.
*** [armv8_crypto_wrap.o] Error code 1

make[4]: stopped in /usr/src/sys/modules/armv8crypto
.ERROR_TARGET='armv8_crypto_wrap.o'
.ERROR_META_FILE='/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG/modules/usr/src/sys/modules/armv8crypto/armv8_crypto_wrap.o.meta'
.MAKE.LEVEL='4'
MAKEFILE=''
.MAKE.MODE='meta missing-filemon=yes missing-meta=yes silent=yes verbose'
_ERROR_CMD='cc -mcpu=cortex-a53 -target aarch64-unknown-freebsd12.0 --sysroot=/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp -B/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/bin -c -O3 -pipe -fno-strict-aliasing -Werror -D_KERNEL -DKLD_MODULE -DHAVE_KERNEL_OPTION_HEADERS -include /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG/opt_global.h -I. -I/usr/src/sys -fno-common -g -fPIC -I/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG -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; ctfconvert -L VERSION -g armv8_crypto_wrap.o;'
.CURDIR='/usr/src/sys/modules/armv8crypto'
.MAKE='make'
.OBJDIR='/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG/modules/usr/src/sys/modules/armv8crypto'
.TARGETS='all'
DESTDIR=''
LD_LIBRARY_PATH=''
MACHINE='arm64'
MACHINE_ARCH='aarch64'
MAKEOBJDIRPREFIX='/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG/modules'
MAKESYSPATH='/usr/src/share/mk'
MAKE_VERSION='20170720'
PATH='/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr/sbin:/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/usr/bin:/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/legacy/bin:/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/sbin:/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/tmp/usr/bin:/sbin:/bin:/usr/sbin:/usr/bin'
SRCTOP='/usr/src'
OBJTOP='/usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG/modules/usr/src'
.MAKE.MAKEFILES='/usr/src/share/mk/sys.mk /usr/src/share/mk/local.sys.env.mk /usr/src/share/mk/src.sys.env.mk /root/src.configs/src.conf.cortexA53dbg-clang-bootstrap.amd64-host /usr/src/share/mk/bsd.mkopt.mk /usr/src/share/mk/bsd.suffixes.mk /root/src.configs/make.conf /usr/src/share/mk/local.sys.mk /usr/src/share/mk/src.sys.mk /dev/null /usr/src/sys/modules/armv8crypto/Makefile /usr/src/share/mk/bsd.kmod.mk /usr/src/sys/conf/kmod.mk /usr/src/share/mk/bsd.init.mk /usr/src/share/mk/bsd.opts.mk /usr/src/share/mk/bsd.cpu.mk /usr/src/share/mk/local.init.mk /usr/src/share/mk/src.init.mk /usr/src/sys/modules/armv8crypto/../Makefile.inc /usr/src/share/mk/bsd.own.mk /usr/src/share/mk/bsd.compiler.mk /usr/src/share/mk/bsd.linker.mk /usr/src/sys/conf/kern.opts.mk /usr/src/sys/conf/config.mk /usr/src/share/mk/bsd.links.mk /usr/src/share/mk/bsd.dep.mk /usr/src/share/mk/bsd.clang-analyze.mk /usr/src/share/mk/bsd.obj.mk /usr/src/share/mk/bsd.subdir.mk /usr/src/sys/conf/kern.mk'
.PATH='. /usr/src/sys/modules/armv8crypto /usr/src/sys/crypto/armv8 /usr/obj/cortexA53dbg_clang/arm64.aarch64/usr/src/sys/GENERIC-DBG'
1 error



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