Date: Sun, 8 Apr 2018 21:51:19 -0700 From: Mark Millard <marklmi26-fbsd@yahoo.com> To: bob prohaska <fbsd@www.zefox.net>, "Rodney W. Grimes" <freebsd-rwg@pdx.rh.CN85.dnsmgr.net>, FreeBSD Current <freebsd-current@freebsd.org> Subject: Re: Module compiles looking in /usr/src when alternate src tree is in use [actually the arm_neon.h and stdint.h issue] Message-ID: <0A2A8AD5-7B99-4E4C-B856-03FB8C61B567@yahoo.com>
next in thread | raw e-mail | index | archive | help
Rodney W. Grimes freebsd-rwg at pdx.rh.CN85.dnsmgr.net wrote on Mon Apr 9 03:54:50 UTC 2018 : > Something for some reason included arm_neon.h? # grep -r arm_neon.h /usr/src/sys/ | more /usr/src/sys/crypto/armv8/armv8_crypto_wrap.c:#include <arm_neon.h> arm_neon.h is something that the kernel source itself has a reference to. [But the stdint.h that was in the error messages was found were the it should not exist as far as I can tell, see below.] # find /usr/src -name .svn -prune -o -name arm_neon.h -print finds nothing. But . . . # find /usr/lib -name arm_neon.h -print /usr/lib/clang/6.0.0/include/arm_neon.h This matches the error message report and is the only copy around in the system areas to find. (Ignoring ports materials and /usr/local/ .) In turn that arm_neon.h has: # grep stdint.h /usr/lib/clang/6.0.0/include/arm_neon.h #include <stdint.h> Looking in a tree that I have (from an amd64 -> arm64 cross build for what is a Cortex-A53 intended use): /usr/obj/DESTDIRs/clang-cortexA53-installworld/ were I did an installworld for arm64: # find /usr/obj/DESTDIRs/clang-cortexA53-installworld -name stdint.h = /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/include/c++/v1/stdint.h= = /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/include/c++/v1/tr1/stdi= nt.h /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/include/sys/stdint.h /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/include/stdint.h There is no stdint.h under that tree's /usr/lib/ area: /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/lib/ was not listed anywhere. For reference relative to arm_neon.h and this tree: # find /usr/obj/DESTDIRs/clang-cortexA53-installworld -name arm_neon.h | = more = /usr/obj/DESTDIRs/clang-cortexA53-installworld/usr/lib/clang/6.0.0/include= /arm_neon.h I conclude that: /usr/lib/clang/6.0.0/include/stdint.h should not have been created in the first place. [Does that stdint.h have file-system dates/times matching the other files from the build? Or does it look to be mismatched and possibly just needs to be deleted?] For reference, all the above is based on source for head -r332293: # uname -apKU FreeBSD FBSDFSSD 12.0-CURRENT FreeBSD 12.0-CURRENT r332293M amd64 = amd64 1200061 1200061 # 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: 332293 Last Changed Rev: 332293 I do not have an arm64 system that is anywhere near up to date at this time so the above evidence is not from a self-hosted build: My context is not a full-match. =3D=3D=3D Mark Millard marklmi26-fbsd at yahoo.com ( dsl-only.net went away in early 2018-Mar)
Want to link to this message? Use this URL: <https://mail-archive.FreeBSD.org/cgi/mid.cgi?0A2A8AD5-7B99-4E4C-B856-03FB8C61B567>