From owner-freebsd-current@freebsd.org Mon Apr 9 05:11:47 2018 Return-Path: Delivered-To: freebsd-current@mailman.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2610:1c1:1:606c::19:1]) by mailman.ysv.freebsd.org (Postfix) with ESMTP id AC16FF800C5 for ; Mon, 9 Apr 2018 05:11:47 +0000 (UTC) (envelope-from marklmi26-fbsd@yahoo.com) Received: from sonic311-23.consmr.mail.gq1.yahoo.com (sonic311-23.consmr.mail.gq1.yahoo.com [98.137.65.204]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 2F21069E9E for ; Mon, 9 Apr 2018 05:11:46 +0000 (UTC) (envelope-from marklmi26-fbsd@yahoo.com) X-YMail-OSG: dQyYg3EVM1mvIrtFYO0JqFgBoMVKSmfxxaCCOH1mTYuHVu_PpVTX5d0.XYC5zPq .IsWtD6rQPOuYmLy0qa2QVtDLIboNpE9vFga9bxSIY2D2z6OQDWjuHK6JyPTo_O7eb2NWGxaO49b 3Btl1qhziWU6bf_Lj.QaRpwgPLACIx8QEauhKQ0BSHbPSngkZLd6UC01l1OXDv_JT9uwNzvzj7nV K_wJdMU0BngeOfrrIlZdhmtJAE8C07ypgcvhMOCPOkzKCuy9yxH7AlkkGxivZWefwhZTZJJKxSwE LJ1_fL29Bc9lRBMa.SqecAMtRnqh3uGsWd25wSK4JOv4nttPE9dAgXoQZYnK_d.MFzqe5.M_CT80 nomGWqc_VKyhLjTJBAHgHPkbW.dSWRwxRRn5Slpl1PGvmlupzDNcLC7duW74Adth2vss1Zg3CzH_ Vm2xmRBpJey7kVx_AFfTUtUgAn4DFUUOv_pnGtlbUnGycNkNk.2sz1Y6cYbkxAxlLooYh0hVHrIG 2ZeBpnD_kzpEIdsZk5PSP_WIFym2c5Y_f8HoObCCQTUEbfmvjhA-- Received: from sonic.gate.mail.ne1.yahoo.com by sonic311.consmr.mail.gq1.yahoo.com with HTTP; Mon, 9 Apr 2018 05:11:40 +0000 Received: from c-76-115-7-162.hsd1.or.comcast.net (EHLO [192.168.1.25]) ([76.115.7.162]) by smtp429.mail.gq1.yahoo.com (Oath Hermes SMTP Server) with ESMTPA ID b2fba2445e6cf2ff6a4bbffc3549ab37; Mon, 09 Apr 2018 04:51:21 +0000 (UTC) From: Mark Millard Content-Type: text/plain; charset=us-ascii Content-Transfer-Encoding: quoted-printable Mime-Version: 1.0 (Mac OS X Mail 11.3 \(3445.6.18\)) 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> Date: Sun, 8 Apr 2018 21:51:19 -0700 To: bob prohaska , "Rodney W. Grimes" , FreeBSD Current X-Mailer: Apple Mail (2.3445.6.18) X-BeenThere: freebsd-current@freebsd.org X-Mailman-Version: 2.1.25 Precedence: list List-Id: Discussions about the use of FreeBSD-current List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 09 Apr 2018 05:11:47 -0000 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 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 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)