From owner-freebsd-arm@freebsd.org Sun Jan 27 01:29:29 2019 Return-Path: Delivered-To: freebsd-arm@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 1FCDB14B7A5C for ; Sun, 27 Jan 2019 01:29:29 +0000 (UTC) (envelope-from ticso@cicely7.cicely.de) Received: from raven.bwct.de (raven.bwct.de [195.149.99.3]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client CN "raven.bwct.de", Issuer "raven.bwct.de" (not verified)) by mx1.freebsd.org (Postfix) with ESMTPS id DA7DA77D75 for ; Sun, 27 Jan 2019 01:29:27 +0000 (UTC) (envelope-from ticso@cicely7.cicely.de) Received: from mail.cicely.de ([10.1.1.37]) by raven.bwct.de (8.15.2/8.15.2) with ESMTPS id x0R1TM7G018627 (version=TLSv1 cipher=DHE-RSA-AES256-SHA bits=256 verify=FAIL); Sun, 27 Jan 2019 02:29:23 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=cicely.de; s=default; t=1548552564; bh=yxCYvGVLEIusb+pOULRVcvLajytsP2CwF2hC23UJYyI=; h=Date:From:To:Cc:Subject:Reply-To:References:In-Reply-To; b=xPyZ9WT55mXXDg/rpLS5syJmvtFjuqe66B+cTm7otDIQ7iC0E5XLTT9Yu9R4hA7uV tP+pMRM2mP7hLRDxVN8dg2V3F799jbfzye2RXNXA2PWGhTrlK2DDcJfdqsTKCwVsmC LiggpYGfw8yUakvEJcq+xwDyElqWVJ6eaf/52ye0= Received: from cicely7.cicely.de (cicely7.cicely.de [10.1.1.9]) by mail.cicely.de (8.14.5/8.14.4) with ESMTP id x0R1Se1G007721 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Sun, 27 Jan 2019 02:28:40 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) Received: from cicely7.cicely.de (localhost [127.0.0.1]) by cicely7.cicely.de (8.15.2/8.15.2) with ESMTP id x0R1Tt9T086453; Sun, 27 Jan 2019 02:29:55 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) Received: (from ticso@localhost) by cicely7.cicely.de (8.15.2/8.15.2/Submit) id x0R1TsVs086452; Sun, 27 Jan 2019 02:29:54 +0100 (CET) (envelope-from ticso) Date: Sun, 27 Jan 2019 02:29:54 +0100 From: Bernd Walter To: Warner Losh Cc: ticso@cicely.de, freebsd-arm@freebsd.org, Bernd Walter Subject: Re: 12-RELEASE loader fails on Orange Pi R1 (maybe 256MB related) Message-ID: <20190127012954.GK74542@cicely7.cicely.de> Reply-To: ticso@cicely.de References: <20190126030330.GI74542@cicely7.cicely.de> <20190126050119.GJ74542@cicely7.cicely.de> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <20190126050119.GJ74542@cicely7.cicely.de> X-Operating-System: FreeBSD cicely7.cicely.de 12.0-STABLE amd64 User-Agent: Mutt/1.5.11 X-Spam-Status: No, score=-2.9 required=4.0 tests=ALL_TRUSTED=-1, BAYES_00=-1.9 autolearn=ham version=3.3.0 X-Spam-Checker-Version: SpamAssassin 3.3.0 (2010-01-18) on spamd.cicely.de X-Rspamd-Queue-Id: DA7DA77D75 X-Spamd-Bar: -- Authentication-Results: mx1.freebsd.org; dkim=pass header.d=cicely.de header.s=default header.b=xPyZ9WT5 X-Spamd-Result: default: False [-2.33 / 15.00]; ARC_NA(0.00)[]; HAS_REPLYTO(0.00)[ticso@cicely.de]; R_DKIM_ALLOW(-0.20)[cicely.de:s=default]; RCVD_COUNT_FIVE(0.00)[5]; FROM_HAS_DN(0.00)[]; RCPT_COUNT_THREE(0.00)[4]; MV_CASE(0.50)[]; NEURAL_HAM_LONG(-0.99)[-0.987,0]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[cicely.de]; REPLYTO_DOM_NEQ_FROM_DOM(0.00)[]; TO_DN_SOME(0.00)[]; TO_MATCH_ENVRCPT_SOME(0.00)[]; DKIM_TRACE(0.00)[cicely.de:+]; MX_GOOD(-0.01)[cached: mx1.bwct.de]; RCVD_IN_DNSWL_NONE(0.00)[3.99.149.195.list.dnswl.org : 127.0.20.0]; NEURAL_HAM_SHORT(-0.58)[-0.578,0]; NEURAL_HAM_MEDIUM(-0.95)[-0.950,0]; R_SPF_NA(0.00)[]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_TLS_LAST(0.00)[]; ASN(0.00)[asn:21461, ipnet:195.149.99.0/24, country:DE]; MID_RHS_MATCH_FROM(0.00)[]; IP_SCORE(-0.00)[country: DE(-0.01)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 27 Jan 2019 01:29:29 -0000 On Sat, Jan 26, 2019 at 06:01:20AM +0100, Bernd Walter wrote: > On Fri, Jan 25, 2019 at 09:36:44PM -0700, Warner Losh wrote: > > On Fri, Jan 25, 2019, 9:08 PM Bernd Walter > > > > > It might be because my R1 is a 256MB, while the tested zero is 512MB. > > > I can test a 256MB zero in a few days, but don't have a 256MB zero at home. > > > > > > > Maybe it is the block cache code? It hovers up a ton of memory.... it was > > fixed on i386, though, I thought... > > Ok, then I will pick up a 256MB Orange Pi zero tomorrow and test with it. Absolutely - it is related to 256MB. This is the same card, which booted on a 512MB zero, now inserted into a 256MB zero: U-Boot SPL 2018.11 (Jan 20 2019 - 22:15:19 +0100) DRAM: 256 MiB Trying to boot from MMC1 U-Boot 2018.11 (Jan 20 2019 - 22:15:19 +0100) Allwinner Technology CPU: Allwinner H3 (SUN8I 1680) Model: Xunlong Orange Pi Zero DRAM: 256 MiB MMC: SUNXI SD/MMC: 0 Loading Environment from FAT... *** Warning - bad CRC, using default environment In: serial Out: serial Err: serial Net: phy interface0 eth0: ethernet@1c30000 starting USB... USB0: USB EHCI 1.00 USB1: USB OHCI 1.0 USB2: USB EHCI 1.00 USB3: USB OHCI 1.0 scanning bus 0 for devices... 1 USB Device(s) found scanning bus 2 for devices... 1 USB Device(s) found scanning usb for storage devices... 0 Storage Device(s) found Hit any key to stop autoboot: 0 switch to partitions #0, OK mmc0 is current device Scanning mmc 0:1... 25259 bytes read in 3 ms (8 MiB/s) Found EFI removable media binary efi/boot/bootarm.efi Scanning disks on usb... Disk usb0 not ready Disk usb1 not ready Disk usb2 not ready Disk usb3 not ready Scanning disks on mmc... MMC Device 1 not found MMC Device 2 not found MMC Device 3 not found Found 3 disks 587736 bytes read in 29 ms (19.3 MiB/s) ## Starting EFI application at 42000000 ... Consoles: EFI console failed to allocate staging area: 14 failed to allocate staging area ## Application terminated, r = 5 EFI LOAD FAILED: continuing... Device 0: device type unknown ... is now current device ethernet@1c30000 Waiting for PHY auto negotiation to complete. done BOOTP broadcast 1 BOOTP broadcast 2 BOOTP broadcast 3 DHCP client bound to address 10.1.1.156 (1045 ms) ... -- B.Walter http://www.bwct.de Modbus/TCP Ethernet I/O Baugruppen, ARM basierte FreeBSD Rechner uvm. From owner-freebsd-arm@freebsd.org Sun Jan 27 01:57:25 2019 Return-Path: Delivered-To: freebsd-arm@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 0042E14B8DDD for ; Sun, 27 Jan 2019 01:57:24 +0000 (UTC) (envelope-from ticso@cicely7.cicely.de) Received: from raven.bwct.de (raven.bwct.de [195.149.99.3]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client CN "raven.bwct.de", Issuer "raven.bwct.de" (not verified)) by mx1.freebsd.org (Postfix) with ESMTPS id EE9AF81001 for ; Sun, 27 Jan 2019 01:57:23 +0000 (UTC) (envelope-from ticso@cicely7.cicely.de) Received: from mail.cicely.de ([10.1.1.37]) by raven.bwct.de (8.15.2/8.15.2) with ESMTPS id x0R1vKhI019232 (version=TLSv1 cipher=DHE-RSA-AES256-SHA bits=256 verify=FAIL); Sun, 27 Jan 2019 02:57:21 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=cicely.de; s=default; t=1548554241; bh=Y5rY1EI+T1DGrapt7WbOCnO7C9+bOC508/K/sI8pRSA=; h=Date:From:To:Cc:Subject:Reply-To:References:In-Reply-To; b=MjgkETvYx0QmCPu4md3prT5gn3IS/p5pQf/91+tbzZVfF4EiVtaDH+wJlqgWjG3/l ZKoo8Ue1jRjny9BUCeuCNAicjs++IoCajRpADTZyorIMYKdr6ml51uB8QjPKVmwikw rX3PdvZDXgf+00OtFVEqqzdgftsDJ7aWVFNcF7eM= Received: from cicely7.cicely.de (cicely7.cicely.de [10.1.1.9]) by mail.cicely.de (8.14.5/8.14.4) with ESMTP id x0R1uc2o008402 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Sun, 27 Jan 2019 02:56:38 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) Received: from cicely7.cicely.de (localhost [127.0.0.1]) by cicely7.cicely.de (8.15.2/8.15.2) with ESMTP id x0R1vr7D086576; Sun, 27 Jan 2019 02:57:53 +0100 (CET) (envelope-from ticso@cicely7.cicely.de) Received: (from ticso@localhost) by cicely7.cicely.de (8.15.2/8.15.2/Submit) id x0R1vrQT086575; Sun, 27 Jan 2019 02:57:53 +0100 (CET) (envelope-from ticso) Date: Sun, 27 Jan 2019 02:57:53 +0100 From: Bernd Walter To: Mark Millard Cc: ticso@cicely.de, freebsd-arm@freebsd.org, Bernd Walter Subject: Re: 12-RELEASE Translation Fault (L1) on some H3 Orange Pi Message-ID: <20190127015753.GM74542@cicely7.cicely.de> Reply-To: ticso@cicely.de References: <20190126023533.GG74542@cicely7.cicely.de> <54D54476-7A53-4458-A847-FDD245052313@yahoo.com> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <54D54476-7A53-4458-A847-FDD245052313@yahoo.com> X-Operating-System: FreeBSD cicely7.cicely.de 12.0-STABLE amd64 User-Agent: Mutt/1.5.11 X-Spam-Status: No, score=-2.9 required=4.0 tests=ALL_TRUSTED=-1, BAYES_00=-1.9 autolearn=ham version=3.3.0 X-Spam-Checker-Version: SpamAssassin 3.3.0 (2010-01-18) on spamd.cicely.de X-Rspamd-Queue-Id: EE9AF81001 X-Spamd-Bar: -- Authentication-Results: mx1.freebsd.org; dkim=pass header.d=cicely.de header.s=default header.b=MjgkETvY X-Spamd-Result: default: False [-2.31 / 15.00]; HAS_REPLYTO(0.00)[ticso@cicely.de]; TO_DN_SOME(0.00)[]; MV_CASE(0.50)[]; DKIM_TRACE(0.00)[cicely.de:+]; MX_GOOD(-0.01)[cached: mx1.bwct.de]; NEURAL_HAM_SHORT(-0.56)[-0.565,0]; FREEMAIL_TO(0.00)[yahoo.com]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_TLS_LAST(0.00)[]; ASN(0.00)[asn:21461, ipnet:195.149.99.0/24, country:DE]; MID_RHS_MATCH_FROM(0.00)[]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-0.95)[-0.948,0]; R_DKIM_ALLOW(-0.20)[cicely.de:s=default]; RCVD_COUNT_FIVE(0.00)[5]; FROM_HAS_DN(0.00)[]; RCPT_COUNT_THREE(0.00)[4]; NEURAL_HAM_LONG(-0.99)[-0.985,0]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[cicely.de]; REPLYTO_DOM_NEQ_FROM_DOM(0.00)[]; TO_MATCH_ENVRCPT_SOME(0.00)[]; RCVD_IN_DNSWL_NONE(0.00)[3.99.149.195.list.dnswl.org : 127.0.20.0]; R_SPF_NA(0.00)[]; IP_SCORE(-0.00)[country: DE(-0.01)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 27 Jan 2019 01:57:25 -0000 On Sat, Jan 26, 2019 at 12:33:54AM -0800, Mark Millard via freebsd-arm wrote: > On 2019-Jan-25, at 18:35, Bernd Walter wrote: > > > On a Plus 2E: > > [270]cicely7# dd if=FreeBSD-12.0-RELEASE-arm-armv7-GENERICSD.img of=/dev/da0 bs=1m > > 3072+0 records in > > 3072+0 records out > > 3221225472 bytes transferred in 41.028696 secs (78511524 bytes/sec) > > [84]cicely7# cd ../u-boot-orangepi-plus-2e/ > > [85]cicely7# dd if=u-boot-sunxi-with-spl.bin of=/dev/da0 bs=1k seek=8 conv=sync > > 401+1 records in > > 402+0 records out > > 411648 bytes transferred in 4.064207 secs (101286 bytes/sec) > > > > ... > > Loading kernel... > > /boot/kernel/kernel text=0x8649ac data=0xb0da0+0x1f58a0 syms=[0x4+0xa1060+0x4+0x101505] > > Loading configured modules... > > /boot/kernel/umodem.ko text=0x1550 text=0xf30 data=0x1080+0xf84 syms=[0x4+0xe90+0x4+0xa7e] > > loading required module 'ucom' > > /boot/kernel/ucom.ko text=0x174c text=0x2a30 data=0x1080+0x17b8 syms=[0x4+0x13e0+0x4+0xbac] > > can't find '/boot/entropy' > > > > Hit [Enter] to boot immediately, or any other key for command prompt. > > Booting [/boot/kernel/kernel]... > > Using DTB provided by EFI at 0x47ef5000. > > EHCI failed to shut down host controller. > > EHCI failed to shut down host controller. > > EHCI failed to shut down host controller. > > EHCI failed to shut down host controller. > > Kernel entry at 0xb1000180... > > Kernel args: (null) > > modulep: 0xc0cc8000 > > relocation_offset 0 > > ---<>--- > > Copyright (c) 1992-2018 The FreeBSD Project. > > Copyright (c) 1979, 1980, 1983, 1986, 1988, 1989, 1991, 1992, 1993, 1994 > > The Regents of the University of California. All rights reserved. > > FreeBSD is a registered trademark of The FreeBSD Foundation. > > FreeBSD 12.0-RELEASE r341666 GENERIC arm > > FreeBSD clang version 6.0.1 (tags/RELEASE_601/final 335540) (based on LLVM 6.0.1) > > . . . > > aw_wdog0: mem 0x1c20ca0-0x1c20cbf irq 25 on simplebus0 > > pcm0: mem 0x1c22c00-0x1c22fff irq 29 on simplebus0 > > Fatal kernel mode data abort: 'Translation Fault (L1)' on read > > trapframe: 0xc0d13bc8 > > FSR=00000005, FAR=00000004, spsr=600000d3 > > r0 =c4ee3a00, r1 =00000000, r2 =00000080, r3 =00000000 > > r4 =c4ee3a00, r5 =c6e7b680, r6 =00000080, r7 =00000000 > > r8 =00000007, r9 =c4ee3a00, r10=ffffffff, r11=c0d13c78 > > r12=00000000, ssp=c0d13c58, slr=c062f92c, pc =c062fa3c > > > > panic: Fatal abort > > cpuid = 0 > > time = 1 > > Uptime: 1s > > > What I did to enable booting an Orange Pi Plus 2E for head > was to build based on: > > # svnlite diff /usr/src/sys/gnu/dts/arm/sun8i-h3-orangepi-pc.dts > Index: /usr/src/sys/gnu/dts/arm/sun8i-h3-orangepi-pc.dts > =================================================================== > --- /usr/src/sys/gnu/dts/arm/sun8i-h3-orangepi-pc.dts (revision 341836) > +++ /usr/src/sys/gnu/dts/arm/sun8i-h3-orangepi-pc.dts (working copy) > @@ -106,7 +106,7 @@ > "Line Out", "LINEOUT", > "MIC1", "Mic", > "Mic", "MBIAS"; > - status = "okay"; > + status = "disabled"; > }; > > &de { > > This avoided the software problem(s) associated but is a > workaround/hack. I'm using 12-RELEASE, but will give this a try. Indeed, the failing boards have microphones, while the other do not. -- B.Walter http://www.bwct.de Modbus/TCP Ethernet I/O Baugruppen, ARM basierte FreeBSD Rechner uvm. From owner-freebsd-arm@freebsd.org Sun Jan 27 17:05:40 2019 Return-Path: Delivered-To: freebsd-arm@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 B048214B502B for ; Sun, 27 Jan 2019 17:05:40 +0000 (UTC) (envelope-from tech-lists@zyxst.net) Received: from out5-smtp.messagingengine.com (out5-smtp.messagingengine.com [66.111.4.29]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 75E947301B for ; Sun, 27 Jan 2019 17:05:38 +0000 (UTC) (envelope-from tech-lists@zyxst.net) Received: from compute4.internal (compute4.nyi.internal [10.202.2.44]) by mailout.nyi.internal (Postfix) with ESMTP id 5842E21AD0 for ; Sun, 27 Jan 2019 12:05:32 -0500 (EST) Received: from mailfrontend1 ([10.202.2.162]) by compute4.internal (MEProxy); Sun, 27 Jan 2019 12:05:32 -0500 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=zyxst.net; h= date:from:to:subject:message-id:mime-version:content-type; s= fm1; bh=o9HLmy5S4bz08PKMmnIYzKn2xd9ddvjitk7RbmFhiS4=; b=KuIkQ3XO PJ6l59Nxa2ovVAPaNvtXwK1MPwXK/tiu/vcWGR8pEIsA9kB0wT6BWBH4JsFdezkr r4/zWz/ppsaZ8InWrjXlLx5SGs1JvJ15DdOfFT41VT6lwOYB7Dtgmv67Zd91y5h2 aEaDwOCBVyB6Nwqr7Lg0BEQhdEW3EvJ9xxt/Bm19ayaqchOQik2f0ZagVdeVmqiQ Z3osKU6XPojiXc8MhMovtrekgXgzkMXpnor8KQwONA3t3eOsnpOTmSR8b4ZF0uLV a5nu5n82GM8C/2lx6Qjx8MZJJBrMl13EkaCX1SVk2xEDZzfp2yo8TfUrxd06JN9G f/tGujkvhaaP7Q== DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d= messagingengine.com; h=content-type:date:from:message-id :mime-version:subject:to:x-me-proxy:x-me-proxy:x-me-sender :x-me-sender:x-sasl-enc; s=fm1; bh=o9HLmy5S4bz08PKMmnIYzKn2xd9dd vjitk7RbmFhiS4=; b=HxiA7121mHgldhXUE4mnGSoF67vbj3NqNYneS3uS5ZE7l wTACDvg0QdLYujGZwtlRcygwfBvDRIB/z1btRnm3IRH9jcz1U8Pf2fkGnjCvc6mP uSKqe99i0lvYBYRiMxZgboAEWn256JD6dNn42UsJuoNf/roCvVK1Ep2A3mf18iPR kHl/pUkDcThKziyMZeV75bnkKg+uBranvaMgTEhk3mJe8rTmQ7+yqFKh5RUOJUno gf6223POiatCOA4OfEms62EjtEErWeSIYhC2L9HKYZdJwAZPeJLDDbA8xaD6wIZq Dtx+O7/eWLRH3uwjnU8yNJVTSlwHK45kKRVIj7Y0g== X-ME-Sender: X-ME-Proxy-Cause: gggruggvucftvghtrhhoucdtuddrgedtledrieekgdeliecutefuodetggdotefrodftvf curfhrohhfihhlvgemucfhrghsthforghilhdpqfhuthenuceurghilhhouhhtmecufedt tdenucenucfjughrpeffhffvuffkgggtuggfsehttdertddtredvnecuhfhrohhmpehtvg gthhdqlhhishhtshcuoehtvggthhdqlhhishhtshesiiihgihsthdrnhgvtheqnecukfhp peekvddrjedtrdeluddruddtudenucfrrghrrghmpehmrghilhhfrhhomhepthgvtghhqd hlihhsthhsseiihiigshhtrdhnvghtnecuvehluhhsthgvrhfuihiivgeptd X-ME-Proxy: Received: from rpi3.zyxst.net (rpi3.zyxst.net [82.70.91.101]) by mail.messagingengine.com (Postfix) with ESMTPA id 77450E41F3 for ; Sun, 27 Jan 2019 12:05:31 -0500 (EST) Date: Sun, 27 Jan 2019 17:05:29 +0000 From: tech-lists To: freebsd-arm@freebsd.org Subject: weird boot problem on rpi3 Message-ID: <20190127170528.GA2096@rpi3.zyxst.net> Mail-Followup-To: freebsd-arm@freebsd.org MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii; format=flowed Content-Disposition: inline User-Agent: Mutt/1.11.2 (2019-01-07) X-Rspamd-Queue-Id: 75E947301B X-Spamd-Bar: ------- Authentication-Results: mx1.freebsd.org; dkim=pass header.d=zyxst.net header.s=fm1 header.b=KuIkQ3XO; dkim=pass header.d=messagingengine.com header.s=fm1 header.b=HxiA7121; spf=pass (mx1.freebsd.org: domain of tech-lists@zyxst.net designates 66.111.4.29 as permitted sender) smtp.mailfrom=tech-lists@zyxst.net X-Spamd-Result: default: False [-7.22 / 15.00]; ARC_NA(0.00)[]; RCVD_VIA_SMTP_AUTH(0.00)[]; R_DKIM_ALLOW(-0.20)[zyxst.net:s=fm1,messagingengine.com:s=fm1]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; FROM_HAS_DN(0.00)[]; R_SPF_ALLOW(-0.20)[+ip4:66.111.4.29]; TO_MATCH_ENVRCPT_ALL(0.00)[]; MIME_GOOD(-0.10)[text/plain]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; TO_DN_NONE(0.00)[]; RCPT_COUNT_ONE(0.00)[1]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; RCVD_COUNT_THREE(0.00)[4]; DMARC_NA(0.00)[zyxst.net]; DKIM_TRACE(0.00)[zyxst.net:+,messagingengine.com:+]; MX_GOOD(-0.01)[in2-smtp.messagingengine.com,in1-smtp.messagingengine.com,in2-smtp.messagingengine.com,in1-smtp.messagingengine.com,in2-smtp.messagingengine.com,in1-smtp.messagingengine.com]; NEURAL_HAM_SHORT(-0.98)[-0.979,0]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_TLS_LAST(0.00)[]; ASN(0.00)[asn:11403, ipnet:66.111.4.0/24, country:US]; IP_SCORE(-3.63)[ip: (-9.71), ipnet: 66.111.4.0/24(-4.70), asn: 11403(-3.65), country: US(-0.08)]; RCVD_IN_DNSWL_LOW(-0.10)[29.4.111.66.list.dnswl.org : 127.0.5.1] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 27 Jan 2019 17:05:40 -0000 Hi, I'm running a headless rpi3 with freebsd-12 r343022. It's self-hosting - by that I mean I've built/installed world/kernel on the device more than once. It has a wifi dongle, a usb-powered hd and a wireless keyboard dongle plugged into the usb ports. It all works great, apart from the following problem: If the rpi3 needs to reboot, it will not come back up again unless the keyboard dongle is plugged in (and the keyboard itself is turned on). It doesn't matter if the other peripherals are plugged in or not. To come back up again, the keyboard must be turned on and its dongle plugged in. It doesn't matter if I use shutdown -r now, poweroff (then unplug/plugin power) or halt then powercycle. I have plugged in a monitor to see where it fails. It fails at the point where a probe to the keyboard would be expected. It just sits there and doesn't proceed. There's no error 'no keyboard detected' or anything like that. How can I fix this? thanks, -- J. From owner-freebsd-arm@freebsd.org Mon Jan 28 08:40:11 2019 Return-Path: Delivered-To: freebsd-arm@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 2686E14ABAD5 for ; Mon, 28 Jan 2019 08:40:11 +0000 (UTC) (envelope-from 5c4ebc79747a44254ef3f716-freebsd+2Darm=freebsd.org@return.mxmail.io) Received: from relay-4.emailamp.com (relay-4.emailamp.com [185.175.161.11]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 5ADE9805B4 for ; Mon, 28 Jan 2019 08:40:10 +0000 (UTC) (envelope-from 5c4ebc79747a44254ef3f716-freebsd+2Darm=freebsd.org@return.mxmail.io) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe; bh=sLNBm59BEX4YZGJ26VTawxZL/3ffed/qISOTDObstDU=; b=ecEazIX0EVNWRmlPfNXYq/swJnYg7npeGUuCkwYXuG2sGSzTKUzSb0RQEgJj4uiSk47uzeVKfDjB 2UASSynt2lLkBeBByDrsBzI4699Rtn9Lm/GwBoma0iPYX+jv5tsPIU8mjAvn/uHcFNKxUx4FvFUs MgoGvu5ux8pcqQmCnK/k9CXxE4y5MOiJ4C9xrYOBqsxZSgNk7UEVC1BQhdQWRJzslRdi8Vi0DofI +HGmPo858ManLJQcSAFOlP93B+gUS/ixQc9wZWxwzQjWUr6WI0PNa4BKTElvnu1rO261TBdzSDyh +RxRcT8SCRCjCgjeeLAFg1vDcTgBu3SzfP4RIg== DKIM-Signature: v=1; a=rsa-sha256; c=simple; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe:From:To:Subject; t=1548664810; x=1548686410; bh=nHiIK0c+E/XQFFpRi1JCByjZe2X0cCvrdKayCxH9t0g=; b=I9r+oNlSwcM+tWIAyK3yhQUtslzG3XuQ1W1gQchOO9bQATUOwJzi26laQNSodis7m4cr6+Pd5iYJ TWRA4oGpdo8LV7F154y1j58tDFAMoJjgVT0yrWOxomcV15s5gMs4rn6paMlQmQh5iQGQzz3u6jt0 cI1BT7y9G0YNYMtodACFzGwSkj5aY6AuwuA0X0O0dzLFLq1i3kmfn1IvsKoMFDruUbFsl5IabCRo P2GqLOl78+28LcoPg1+BI3rj5FOvzly0NZ6TrbHH8nElHauX1mX7XSo3EOJkRDyCG6S7WskHcFmJ ZvDxuQGxuNBVelFd0eIl8OUyg5ByWKWPu+K+/Q== Received: by mx-out-gi2.emailamp.com id h9qvuk2em8c9 for ; Mon, 28 Jan 2019 03:26:06 -0500 (envelope-from <5c4ebc79747a44254ef3f716-freebsd+2Darm=freebsd.org@return.mxmail.io>) Date: Mon, 28 Jan 2019 10:26:06 +0200 Subject: Riverside apartments 🏡 in UK hipster capital To: freebsd-arm@freebsd.org From: "Prop Investors Club" Reply-To: Message-Id: List-Unsubscribe-Post: List-Unsubscribe=One-Click Bounces-to: 5c4ebc79747a44254ef3f716@return.mxmail.io X-Auto-Response-Suppress: All Original-from: reply@propinvestors.club Precedence: Bulk X-SES-CONFIGURATION-SET: mxm X-Rspamd-Queue-Id: 5ADE9805B4 X-Spamd-Bar: ++++++++ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=emailamp.com header.s=email header.b=ecEazIX0; dkim=pass header.d=emailamp.com header.s=email header.b=I9r+oNlS; dmarc=fail reason="" header.from=propinvestors.club (policy=none) X-Spamd-Result: default: False [8.11 / 15.00]; HAS_REPLYTO(0.00)[reply@propinvestors.club]; ZERO_FONT(1.00)[23]; TO_DN_NONE(0.00)[]; REPLYTO_ADDR_EQ_FROM(0.00)[]; DKIM_TRACE(0.00)[emailamp.com:+]; MX_GOOD(-0.01)[cached: return.mxmail.io]; FORGED_SENDER(0.30)[reply@propinvestors.club,5c4ebc79747a44254ef3f716-freebsd@return.mxmail.io]; RCVD_TLS_LAST(0.00)[]; IP_SCORE(0.73)[ip: (1.02), ipnet: 185.175.160.0/22(0.73), asn: 9009(1.98), country: GB(-0.09)]; ASN(0.00)[asn:9009, ipnet:185.175.160.0/22, country:GB]; TAGGED_FROM(0.00)[2Darm=freebsd.org]; FROM_NEQ_ENVFROM(0.00)[reply@propinvestors.club,5c4ebc79747a44254ef3f716-freebsd@return.mxmail.io]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[emailamp.com:s=email]; MID_RHS_MATCH_FROM(0.00)[]; FROM_HAS_DN(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; PRECEDENCE_BULK(0.00)[]; SUBJECT_NEEDS_ENCODING(1.00)[]; R_BAD_CTE_7BIT(1.05)[7bit,utf8]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; HAS_LIST_UNSUB(-0.01)[]; RCPT_COUNT_ONE(0.00)[1]; MANY_INVISIBLE_PARTS(1.00)[10]; NEURAL_SPAM_SHORT(0.96)[0.958,0]; NEURAL_SPAM_MEDIUM(1.00)[1.000,0]; NEURAL_SPAM_LONG(1.00)[1.000,0]; MIME_HTML_ONLY(0.20)[]; R_SPF_NA(0.00)[]; RCVD_COUNT_TWO(0.00)[2]; GREYLIST(0.00)[pass,body]; DMARC_POLICY_SOFTFAIL(0.10)[propinvestors.club : No valid SPF, DKIM not aligned (relaxed), none] X-Spam: Yes MIME-Version: 1.0 Content-Type: text/plain; charset="utf-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 28 Jan 2019 08:40:11 -0000 From owner-freebsd-arm@freebsd.org Tue Jan 29 07:50:54 2019 Return-Path: Delivered-To: freebsd-arm@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 23D8114AFB8D for ; Tue, 29 Jan 2019 07:50:54 +0000 (UTC) (envelope-from 5c500595747a44254efad8ce-freebsd+2Darm=freebsd.org@return.mxmail.io) Received: from relay-3.emailamp.com (relay-3.emailamp.com [185.175.161.10]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 238AB70F02 for ; Tue, 29 Jan 2019 07:50:48 +0000 (UTC) (envelope-from 5c500595747a44254efad8ce-freebsd+2Darm=freebsd.org@return.mxmail.io) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe; bh=w97slAKJh/Lcc8cbXZxquGsu0AvvVHWYMczgiQfIj1g=; b=KzKBq4oAzymmjJUhG8kom74jNg0DaFAIFZ4YAJzSI1TOU3urmYGy+uGCx9rckBMgYWwTkMaUyLCM YbI/ITzulgXUElO4PUabVfnFYWKL1vXxc02f4QlTqsmgA1faW6kyxGIdasEDNQp9NZdNHUvFIok8 PngfGemlRRM1hPkmbtwoB2AGj/Fh2e5wmzG9vcH/toSsBAl1r70oixZkFzKN8zAh/eV6B+ZE8Lum R0m3sZFgHuPivnARdumf4RKiyAz+Aze1BY525vdWB2+HVsMrjZ9qE/boL85RWKhJB9ScroEUxzCO WWBhKe7xxByxxmdvZHEltn/aet5qAEYShl06DA== DKIM-Signature: v=1; a=rsa-sha256; c=simple; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe:From:To:Subject; t=1548748249; x=1548769849; bh=KGEfyJ97EjA0kmbPqpkL7Pk5o0w61URqw2T5qt55KOI=; b=S8/rNuU6sbPjAleOm6RGSkNSnQ8cvf8kinsub6PaDzN0tIZmCi8FJk4Bp2oM6RJaZX4KZOa23Xpe bNOHCOYhQflS3xkSktE+apE7yZR1YuGlNQC+yA46Dvtt6p5PLNmgDDvYwZJ86zzpnySPXdEPNnr0 9ShuaMul88TPDHrqHX00l3KoJ8Rh7pAbwmkfhZNwi0F7eSi3dOheOUegw3UU3PIUQR+qCeyViRSL hi7milG5SFFWj9ZWmRj/WkxYsGWfKD37wUHMkubk3qtsyB1GKo7c8Z8r0RNyVyflfOr3Q0cDJmb2 iintelNQFBNVJwb4jGG8bAb94kMR8HaTsaHC3A== Received: by mx-out-gi2.emailamp.com id ha02ti2em8c8 for ; Tue, 29 Jan 2019 02:50:20 -0500 (envelope-from <5c500595747a44254efad8ce-freebsd+2Darm=freebsd.org@return.mxmail.io>) Date: Tue, 29 Jan 2019 09:50:20 +0200 Subject: Care home sector still strong and stable To: freebsd-arm@freebsd.org From: "Prop Investors Club" Reply-To: Message-Id: List-Unsubscribe-Post: List-Unsubscribe=One-Click Bounces-to: 5c500595747a44254efad8ce@return.mxmail.io X-Auto-Response-Suppress: All Original-from: reply@propinvestors.club Precedence: Bulk X-SES-CONFIGURATION-SET: mxm X-Rspamd-Queue-Id: 238AB70F02 X-Spamd-Bar: ++++++ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=emailamp.com header.s=email header.b=KzKBq4oA; dkim=pass header.d=emailamp.com header.s=email header.b=S8/rNuU6; dmarc=fail reason="" header.from=propinvestors.club (policy=none) X-Spamd-Result: default: False [6.90 / 15.00]; HAS_REPLYTO(0.00)[reply@propinvestors.club]; ZERO_FONT(1.00)[21]; TO_DN_NONE(0.00)[]; REPLYTO_ADDR_EQ_FROM(0.00)[]; DKIM_TRACE(0.00)[emailamp.com:+]; MX_GOOD(-0.01)[cached: return.mxmail.io]; FORGED_SENDER(0.30)[reply@propinvestors.club,5c500595747a44254efad8ce-freebsd@return.mxmail.io]; RCVD_TLS_LAST(0.00)[]; IP_SCORE(0.49)[ipnet: 185.175.160.0/22(0.64), asn: 9009(1.90), country: GB(-0.09)]; ASN(0.00)[asn:9009, ipnet:185.175.160.0/22, country:GB]; MID_RHS_MATCH_FROM(0.00)[]; TAGGED_FROM(0.00)[2Darm=freebsd.org]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[emailamp.com:s=email]; FROM_NEQ_ENVFROM(0.00)[reply@propinvestors.club,5c500595747a44254efad8ce-freebsd@return.mxmail.io]; FROM_HAS_DN(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; PRECEDENCE_BULK(0.00)[]; R_BAD_CTE_7BIT(1.05)[7bit,utf8]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; HAS_LIST_UNSUB(-0.01)[]; RCPT_COUNT_ONE(0.00)[1]; MANY_INVISIBLE_PARTS(1.00)[10]; NEURAL_SPAM_SHORT(0.98)[0.984,0]; NEURAL_SPAM_MEDIUM(1.00)[1.000,0]; NEURAL_SPAM_LONG(1.00)[1.000,0]; MIME_HTML_ONLY(0.20)[]; R_SPF_NA(0.00)[]; RCVD_COUNT_TWO(0.00)[2]; DMARC_POLICY_SOFTFAIL(0.10)[propinvestors.club : No valid SPF, DKIM not aligned (relaxed), none] X-Spam: Yes MIME-Version: 1.0 Content-Type: text/plain; charset="utf-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 29 Jan 2019 07:50:54 -0000 From owner-freebsd-arm@freebsd.org Tue Jan 29 10:03:40 2019 Return-Path: Delivered-To: freebsd-arm@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 442DE14B577A for ; Tue, 29 Jan 2019 10:03:40 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from mxrelay.ysv.freebsd.org (mxrelay.ysv.freebsd.org [IPv6:2001:1900:2254:206a::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.ysv.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id D0E17767D1 for ; Tue, 29 Jan 2019 10:03:39 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org (kenobi.freebsd.org [IPv6:2001:1900:2254:206a::16:76]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.ysv.freebsd.org (Postfix) with ESMTPS id 20E7810AF9 for ; Tue, 29 Jan 2019 10:03:39 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org ([127.0.1.118]) by kenobi.freebsd.org (8.15.2/8.15.2) with ESMTP id x0TA3dwc027097 for ; Tue, 29 Jan 2019 10:03:39 GMT (envelope-from bugzilla-noreply@freebsd.org) Received: (from www@localhost) by kenobi.freebsd.org (8.15.2/8.15.2/Submit) id x0TA3dTl027096 for freebsd-arm@FreeBSD.org; Tue, 29 Jan 2019 10:03:39 GMT (envelope-from bugzilla-noreply@freebsd.org) X-Authentication-Warning: kenobi.freebsd.org: www set sender to bugzilla-noreply@freebsd.org using -f From: bugzilla-noreply@freebsd.org To: freebsd-arm@FreeBSD.org Subject: [Bug 179532] wireless networking on ARM Date: Tue, 29 Jan 2019 10:03:39 +0000 X-Bugzilla-Reason: AssignedTo X-Bugzilla-Type: changed X-Bugzilla-Watch-Reason: None X-Bugzilla-Product: Base System X-Bugzilla-Component: arm X-Bugzilla-Version: unspecified X-Bugzilla-Keywords: X-Bugzilla-Severity: Affects Only Me X-Bugzilla-Who: avos@freebsd.org X-Bugzilla-Status: Closed X-Bugzilla-Resolution: FIXED X-Bugzilla-Priority: Normal X-Bugzilla-Assigned-To: freebsd-arm@FreeBSD.org X-Bugzilla-Flags: X-Bugzilla-Changed-Fields: bug_status cc resolution Message-ID: In-Reply-To: References: Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: https://bugs.freebsd.org/bugzilla/ Auto-Submitted: auto-generated MIME-Version: 1.0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 29 Jan 2019 10:03:40 -0000 https://bugs.freebsd.org/bugzilla/show_bug.cgi?id=3D179532 Andriy Voskoboinyk changed: What |Removed |Added ---------------------------------------------------------------------------- Status|Open |Closed CC| |avos@freebsd.org Resolution|--- |FIXED --- Comment #5 from Andriy Voskoboinyk --- Fixed in base r253756. --=20 You are receiving this mail because: You are the assignee for the bug.= From owner-freebsd-arm@freebsd.org Wed Jan 30 07:17:01 2019 Return-Path: Delivered-To: freebsd-arm@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 F023114B6F05 for ; Wed, 30 Jan 2019 07:17:00 +0000 (UTC) (envelope-from 5c514ec8747a44254efd067e-freebsd+2Darm=freebsd.org@return.mxmail.io) Received: from relay-6.emailamp.com (relay-6.emailamp.com [185.175.162.11]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 9402885948 for ; Wed, 30 Jan 2019 07:16:59 +0000 (UTC) (envelope-from 5c514ec8747a44254efd067e-freebsd+2Darm=freebsd.org@return.mxmail.io) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe; bh=VLNxMzyxzPwmL/+VZQkrwqcOkwMrjoiVqtFc48vndII=; b=G5vvuonUS0nUbasRBscDaLATwfJ3JUkuOXVIsPlFbloioo9nlT51Jpvvdy1Av1vVKwma49ShF8Hu CL1VDcLF7zpo+ONCrHeTcj5MYxLsqOR+Znek7V+Dgpn+SZF8liD8wh+m3SOHp+sVvZ8s1CkTo12/ dk8HCpl17ejXg/BP9TtgX4IOkRBvp7z8XPwFlEAzenaZFRiO+av+puvfa7nMNTGgH+dEDwYT198d ig1xaN6HGcVWOixzO6fj8Fz8wRG35gEw03RekrDKxXyPANNpJQ526vLdObkxeCOCKQ7IkJ0m/rwf 9EAdnWVx0o28WxFLLUQqyffEG9QwQcZxWPTgcw== DKIM-Signature: v=1; a=rsa-sha256; c=simple; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe:From:To:Subject; t=1548832619; x=1548854219; bh=yvh8hUsCkwFhqVvJYLaINeoficq48+dDeuSdNj0e8QI=; b=PPQ14raFguwtsLo4vyCMS6iROM5RHrc+Hg4J1ys0Su1tDX86qLa6q3T18Y7jmENAkXggoXiW6pl1 ZsjulyDwolsgVyDzt+BD+pTc+4Z7AcJ9zmtlApYBNqW1Z5JGqrc4N6jf558+IlstQxBcEmn/vPx2 3jAqDndvSrpS5jgqcLBBikdGA/THcfdTaCSBpu4213MGqDUcDjaRsRWQESVC8WobxG3K4vNJCeax kLfEOtCxz/+1j3mB3E+x4qiMTlhv3F16Jv52R5kNBoig44sW+f/y7NVRkr0wGgpMajrZfoYPz7pR 0osHfRPGLXaxpFiC61k9CDUFrBjRoovpEyM4+A== Received: by mx-out-gi2.emailamp.com id ha57mm2em8c7 for ; Wed, 30 Jan 2019 02:15:10 -0500 (envelope-from <5c514ec8747a44254efd067e-freebsd+2Darm=freebsd.org@return.mxmail.io>) Date: Wed, 30 Jan 2019 09:15:10 +0200 Subject: Trafford Plaza is a bold new concept for a bold new generation To: freebsd-arm@freebsd.org From: "Prop Investors Club" Reply-To: Message-Id: List-Unsubscribe-Post: List-Unsubscribe=One-Click Bounces-to: 5c514ec8747a44254efd067e@return.mxmail.io X-Auto-Response-Suppress: All Original-from: reply@propinvestors.club Precedence: Bulk X-SES-CONFIGURATION-SET: mxm X-Rspamd-Queue-Id: 9402885948 X-Spamd-Bar: +++++ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=emailamp.com header.s=email header.b=G5vvuonU; dkim=pass header.d=emailamp.com header.s=email header.b=PPQ14raF; dmarc=fail reason="" header.from=propinvestors.club (policy=none) X-Spamd-Result: default: False [5.66 / 15.00]; HAS_REPLYTO(0.00)[reply@propinvestors.club]; TO_DN_NONE(0.00)[]; REPLYTO_ADDR_EQ_FROM(0.00)[]; DKIM_TRACE(0.00)[emailamp.com:+]; MX_GOOD(-0.01)[cached: return.mxmail.io]; FORGED_SENDER(0.30)[reply@propinvestors.club,5c514ec8747a44254efd067e-freebsd@return.mxmail.io]; RCVD_TLS_LAST(0.00)[]; IP_SCORE(0.79)[ip: (1.62), ipnet: 185.175.160.0/22(0.57), asn: 9009(1.86), country: GB(-0.09)]; ASN(0.00)[asn:9009, ipnet:185.175.160.0/22, country:GB]; MID_RHS_MATCH_FROM(0.00)[]; TAGGED_FROM(0.00)[2Darm=freebsd.org]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[emailamp.com:s=email]; FROM_NEQ_ENVFROM(0.00)[reply@propinvestors.club,5c514ec8747a44254efd067e-freebsd@return.mxmail.io]; FROM_HAS_DN(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; PRECEDENCE_BULK(0.00)[]; HTML_SHORT_LINK_IMG_2(1.00)[]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; HAS_LIST_UNSUB(-0.01)[]; RCPT_COUNT_ONE(0.00)[1]; MANY_INVISIBLE_PARTS(0.50)[6]; NEURAL_SPAM_SHORT(0.99)[0.985,0]; NEURAL_SPAM_MEDIUM(1.00)[1.000,0]; NEURAL_SPAM_LONG(1.00)[1.000,0]; MIME_HTML_ONLY(0.20)[]; R_SPF_NA(0.00)[]; RCVD_COUNT_TWO(0.00)[2]; DMARC_POLICY_SOFTFAIL(0.10)[propinvestors.club : No valid SPF, DKIM not aligned (relaxed), none] MIME-Version: 1.0 Content-Type: text/plain; charset="utf-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 30 Jan 2019 07:17:01 -0000 From owner-freebsd-arm@freebsd.org Wed Jan 30 17:03:06 2019 Return-Path: Delivered-To: freebsd-arm@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 945EE14C69F9 for ; Wed, 30 Jan 2019 17:03:06 +0000 (UTC) (envelope-from doc.solo@web.de) Received: from mout.web.de (mout.web.de [212.227.15.14]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "mout.web.de", Issuer "TeleSec ServerPass DE-2" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 14E8F741D9 for ; Wed, 30 Jan 2019 17:03:04 +0000 (UTC) (envelope-from doc.solo@web.de) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=web.de; s=dbaedf251592; t=1548867782; bh=ToyL+DyWKyM9VwGum8frAYQA6Tsfn9jenSFaznZP28c=; h=X-UI-Sender-Class:From:To:Subject:Date; b=CT6CbkfgyXY7o0T7pCk6eVNkDx4PTJNxL3fD7sF1wnU4noyVg3pP7Sals3gJZ+GVX w2CCWbgWfgbE1AWsgdnVOK7rZDk8QOkm0KNdD4RwyMG0kWWkNMgGrxvMIPZDMwMOR8 Av1JB519K/0Sa/PMCbDEQjQ8oJLvR1+sLE5EiI+Y= X-UI-Sender-Class: c548c8c5-30a9-4db5-a2e7-cb6cb037b8f9 Received: from [95.208.153.190] ([95.208.153.190]) by web-mail.web.de (3c-app-webde-bs03.server.lan [172.19.170.3]) (via HTTP); Wed, 30 Jan 2019 17:57:51 +0100 MIME-Version: 1.0 Message-ID: From: doc.solo@web.de To: freebsd-arm@freebsd.org Subject: Help getting Marvell-A388 SBC booted Content-Type: text/plain; charset=UTF-8 Date: Wed, 30 Jan 2019 17:57:51 +0100 Importance: normal Sensitivity: Normal Content-Transfer-Encoding: quoted-printable X-Priority: 3 X-Provags-ID: V03:K1:LWtfc3CaZ+LPF9gsEzkAjvvo6rf/GWSi8D9VgVVwdHJ/6fOEtAYNsE236qjKdW/Tplvkc 8hOzMuXEtOoqge939oT8Q8JyHm7h1/Tu26WU2JSF5XN36TUm2sz1pzqS638ADJPTPlx/yCnQJmhR AcUrvQPn1lkfIJ3xI6iu3OQtqrNesuHQW7fcWEEiLf+XtkFYVvhcJzMJMBbIXCtA4rjQxP79mR9T C3rxwQySGbw1+EWlctkwYdHNc+7meIS1kWHxOcA5gA45uy2G/DXmHA0oNVMFtvHaD8yfA8Z0x7tz 7Q= X-Spam-Flag: NO X-UI-Out-Filterresults: notjunk:1;V03:K0:zJl2Ns3TA5E=:LM41sTHwGXZ0y0+rD65pKH NRMYqnWt06mFtlJTm6AuixDzndz17LW45m/Mgij3dkxEzpf0wdqHLr0MFtXwHte+6ocZSJGr4 ETFTvQDAxw/g0T7OQ7VUtyJHLK4kmFc1Ubn0vJkcHEsOb1jzah/gl3WTG3R0OlrT/MFtyJMjr /KoddXTTJYk+J7y1/PIHMXwdva7zPudo06Gf+mmJgTM4HrkaxVNeyZxNwcOBcrrfmRgwsz0yJ LRlK/luxpf4RklP08Ehnr4Q2N6/SSwZQyOvr1MHys7yxfAVOsXSSJo/NWFWHAD5KtSS8zLabD +zxIXI5YDw/WDrX8zrseu6crS++7GcgI5uOW0HlYmScKduUJStdKAaqQ1+HxLqY3vuo9qo/3L ysI+jgOTkSsVn+4UFj/SQuNgp6k1b8VHJthaKA33WWefFVlPSmXBvFwbpcv+VW5vBf6bozH6E 1NxP4707OAFUnV42VCV1ysr+fNeyYwVI5PDGa1caKZ+KQ/MFgsHGgeiPjrJ3/NXvNNOiA3/ZP xkxUGwqV1JUk8PWtxQqEZRGY3E5usTOSh8gp58iCrwPNbI38npmK4z1qaL/C87yqvk2tnkJdl Bi0RRVHiYYiBk= X-Rspamd-Queue-Id: 14E8F741D9 X-Spamd-Bar: / Authentication-Results: mx1.freebsd.org; dkim=pass header.d=web.de header.s=dbaedf251592 header.b=CT6Cbkfg; spf=pass (mx1.freebsd.org: domain of doc.solo@web.de designates 212.227.15.14 as permitted sender) smtp.mailfrom=doc.solo@web.de X-Spamd-Result: default: False [-0.40 / 15.00]; R_SPF_ALLOW(-0.20)[+ip4:212.227.15.0/25]; FREEMAIL_FROM(0.00)[web.de]; TO_DN_NONE(0.00)[]; DKIM_TRACE(0.00)[web.de:+]; MX_GOOD(-0.01)[mx-ha02.web.de,mx-ha03.web.de]; HAS_X_PRIO_THREE(0.00)[3]; RECEIVED_SPAMHAUS_PBL(0.00)[190.153.208.95.zen.spamhaus.org : 127.0.0.10]; RCVD_IN_DNSWL_LOW(-0.10)[14.15.227.212.list.dnswl.org : 127.0.5.1]; MIME_TRACE(0.00)[0:+]; FROM_EQ_ENVFROM(0.00)[]; ASN(0.00)[asn:8560, ipnet:212.227.0.0/16, country:DE]; FREEMAIL_ENVFROM(0.00)[web.de]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-0.33)[-0.331,0]; R_DKIM_ALLOW(-0.20)[web.de:s=dbaedf251592]; RCVD_TLS_LAST(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; NEURAL_HAM_LONG(-0.05)[-0.053,0]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[web.de]; RCPT_COUNT_ONE(0.00)[1]; DWL_DNSWL_LOW(-1.00)[web.de.dwl.dnswl.org : 127.0.5.1]; IP_SCORE(0.27)[ipnet: 212.227.0.0/16(-0.74), asn: 8560(2.11), country: DE(-0.01)]; NEURAL_SPAM_SHORT(0.82)[0.822,0]; FROM_NO_DN(0.00)[]; MID_RHS_NOT_FQDN(0.50)[]; RCVD_COUNT_TWO(0.00)[2] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 30 Jan 2019 17:03:06 -0000 Hi, I'm trying to get FreeBSD-12 booted on this device: https://wiki=2Ekobol= =2Eio/ It's a Marvell-A388 based SBC=2E No matter what I tried, I got this output: --- Autoboot in 0 seconds, hit [Enter] to boot or any other key to stop = =20 Loading kernel=2E=2E=2E /boot/kernel/kernel text=3D0x864d6c data=3D0xb0da0+0x1f54e0 syms=3D[0x4+0x= a1060+0x4+0x101505] Loading configured modules=2E=2E=2E can't find '/boot/entropy' Using DTB provided by U-Boot at address 0x2040000=2E Kernel entry at 0x2400180=2E=2E=2E Kernel args: (null) --- No error message, nothing=2E I tried several U-Boot-versions, different pa= rameters, loading addresses=2E The U-Boot part seems to work just fine=2E I= think its ubldr that doesn't get the kernel loaded properly=2E Do I need the FreeBSD specific U-Boot from ports? What makes them special?= What does ubldr need to load the kernel? What should I try to debug any fu= rther? Thanks for your help=2E Regards, S=C3=B6ren=20 From owner-freebsd-arm@freebsd.org Wed Jan 30 22:07:01 2019 Return-Path: Delivered-To: freebsd-arm@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 A5923131A84B for ; Wed, 30 Jan 2019 22:07:01 +0000 (UTC) (envelope-from russ.haley@gmail.com) Received: from mail-io1-xd33.google.com (mail-io1-xd33.google.com [IPv6:2607:f8b0:4864:20::d33]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "smtp.gmail.com", Issuer "Google Internet Authority G3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id DAB6287E2F for ; Wed, 30 Jan 2019 22:07:00 +0000 (UTC) (envelope-from russ.haley@gmail.com) Received: by mail-io1-xd33.google.com with SMTP id b16so963507ior.1 for ; Wed, 30 Jan 2019 14:07:00 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20161025; h=mime-version:from:date:message-id:subject:to; bh=l99rV2KgxUWxF3VOhjp9YDhnasVTSQuyQGi49dcTi1A=; b=O/w7n9LhAeutIr/qYcTShHWAA+56gRWkW02Avu+Wh1Enn9YHQO6Z6DoGLnnOEIIvXY DvuDIZo4sOsHZ+JzW6yFTZVqvRVcSUB46rMYz7ouzZw2A2KiOWC6GoqbxKgrU65zH0xN /9a8WO1EZffxI1ZBoW001RAHCk7gRNBL6cCo2seFkQTR7sz2FdWwWJW8RWYj3ONBH/u5 WxehRsDT1T9FkF4fNGK/0uSMpXgbUEQaNWGovuCcU/4FULrCJZ8oXPGvlmAbHj4C8Gwz n5o9lQXLnh+KcXxn91kyfTwkQzr2imNXdiFBMe36IJbP6RzNtR6xeQk4V0MTODEg7l57 e74g== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:mime-version:from:date:message-id:subject:to; bh=l99rV2KgxUWxF3VOhjp9YDhnasVTSQuyQGi49dcTi1A=; b=CjXrm4TBil//jVnJmOmcp4g28t6mGiQLDJ6OJ5q3wJbwONB2n4881PHqGeajhIKqsK 1eM0z3YvbSeSMlsHYRGoMj9VHku86tpYfUXjHeyYTsKIhYKqen4EPYGSlG8B/c+D1iym 47vvC4WOuH8co+ROiQ00pcqNE04b8mXP/TZGb4adilVLZPdhLq+ZNo+j88QaeH82WbEs kGaGlZeFUDWDbajhX8Mwjt6rKjeNtzLS6FfbILFa2mhDFZe56mR9ezsklN5tsJ1BHANp jWp0Fb/iqmP2UahTGr/puoUawpXfqPkR/r5OqiZ49KXSQP4lRrGT+sOuYqVUKa53pUvH 7Ttw== X-Gm-Message-State: AHQUAuZdGm0Y06iKlgMVdHaBhsZPKU8l58qMcYHwnzwPDonOgaFQaAZN 4K7MC2mI7C/aFLNmK73bT0ugseXSp+pOmch4PsUYHA== X-Google-Smtp-Source: AHgI3IbP+jv03CAHlCW5+rYrf5nC+zjH7DAC7p6sPo97aBdZ86aUo1L/kCtnVvrulOkHoRtmta3D+9LBlzXKbFVho5E= X-Received: by 2002:a5d:94c7:: with SMTP id y7mr17998896ior.285.1548886019926; Wed, 30 Jan 2019 14:06:59 -0800 (PST) MIME-Version: 1.0 From: Russell Haley Date: Wed, 30 Jan 2019 14:06:48 -0800 Message-ID: Subject: Auto expanding filesystem To: freebsd-arm X-Rspamd-Queue-Id: DAB6287E2F X-Spamd-Bar: ------ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=gmail.com header.s=20161025 header.b=O/w7n9Lh; dmarc=pass (policy=none) header.from=gmail.com; spf=pass (mx1.freebsd.org: domain of russhaley@gmail.com designates 2607:f8b0:4864:20::d33 as permitted sender) smtp.mailfrom=russhaley@gmail.com X-Spamd-Result: default: False [-6.68 / 15.00]; R_SPF_ALLOW(-0.20)[+ip6:2607:f8b0:4000::/36]; FREEMAIL_FROM(0.00)[gmail.com]; TO_DN_ALL(0.00)[]; DKIM_TRACE(0.00)[gmail.com:+]; DMARC_POLICY_ALLOW(-0.50)[gmail.com,none]; MX_GOOD(-0.01)[cached: alt3.gmail-smtp-in.l.google.com]; NEURAL_HAM_SHORT(-0.99)[-0.990,0]; FROM_EQ_ENVFROM(0.00)[]; RCVD_TLS_LAST(0.00)[]; MIME_TRACE(0.00)[0:+,1:+]; FREEMAIL_ENVFROM(0.00)[gmail.com]; ASN(0.00)[asn:15169, ipnet:2607:f8b0::/32, country:US]; TAGGED_FROM(0.00)[]; DWL_DNSWL_NONE(0.00)[gmail.com.dwl.dnswl.org : 127.0.5.0]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; R_DKIM_ALLOW(-0.20)[gmail.com:s=20161025]; FROM_HAS_DN(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; MIME_GOOD(-0.10)[multipart/alternative,text/plain]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; RCPT_COUNT_ONE(0.00)[1]; IP_SCORE(-2.67)[ip: (-8.81), ipnet: 2607:f8b0::/32(-2.53), asn: 15169(-1.96), country: US(-0.07)]; RCVD_IN_DNSWL_NONE(0.00)[3.3.d.0.0.0.0.0.0.0.0.0.0.0.0.0.0.2.0.0.4.6.8.4.0.b.8.f.7.0.6.2.list.dnswl.org : 127.0.5.0]; RCVD_COUNT_TWO(0.00)[2] Content-Type: text/plain; charset="UTF-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 30 Jan 2019 22:07:02 -0000 Hi, I was wondering how the auto-expanding filesystem on the FreeBSD provided arm images works? An RTFM link or link to code would be great. I just a thread to pull on as I don't even know where to start. Thanks, Russ From owner-freebsd-arm@freebsd.org Thu Jan 31 07:09:19 2019 Return-Path: Delivered-To: freebsd-arm@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 A7C3F1348F16 for ; Thu, 31 Jan 2019 07:09:19 +0000 (UTC) (envelope-from melounmichal@gmail.com) Received: from mail-wm1-x335.google.com (mail-wm1-x335.google.com [IPv6:2a00:1450:4864:20::335]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "smtp.gmail.com", Issuer "Google Internet Authority G3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 57ED0741D3 for ; Thu, 31 Jan 2019 07:09:18 +0000 (UTC) (envelope-from melounmichal@gmail.com) Received: by mail-wm1-x335.google.com with SMTP id y8so1288261wmi.4 for ; Wed, 30 Jan 2019 23:09:18 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20161025; h=sender:from:reply-to:subject:to:references:openpgp:autocrypt :message-id:date:user-agent:mime-version:in-reply-to :content-language:content-transfer-encoding; bh=XqXF0lsb2rKgYwAxqVkItz7Mvy6loFn2o64ikOyF8oo=; b=jEZ8CcRU3TMROepBzaqEQNY/AkLtK7wgNuYOHD7BgfK+boX/zdOOmKSX9m8TaF0w+h kydyZEemZnMBEMmpEB+DHqYKrofn0Yg4xlOv0YUl2o4a+QGiBC3G+GRdL7rRkguX6tXN mBbue1kCwjIjbPTCuD6NYSxmsa4tAwfI6vz2PpqGguc1UkeFzrFUA9l88zRvAibWjwZh StMxTTCdB1mBHlhAGTFFF1Jcbmq/Ol9LiXOIiOXPfpIJDX9iF7kWZklr7KL6ox1oRLSg V5XY7cxsMdch63y+aBfELKlU/TLe/GLdYRpihUsv/FiuaWafI/HJZK+aAFSzD1F1tnu0 JL4w== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:sender:from:reply-to:subject:to:references :openpgp:autocrypt:message-id:date:user-agent:mime-version :in-reply-to:content-language:content-transfer-encoding; bh=XqXF0lsb2rKgYwAxqVkItz7Mvy6loFn2o64ikOyF8oo=; b=k5954yya2p2ZJzIynjUVl1KHH0r/09YgxQsDUnyMEB6q71goxPDvrY166wcGDrVXZp c0V01Ehm3NASK3tuD400EY/DlXlkeAuIfPW1fzBQ25/8NBwnO9rnM/JI48To15Nwp4gM LdH0okjLFsTcbdVBNzlBc8RR5rBr8MjGkdFVu7F0Tb4X+3b8AdKGcC1aLmhdFF49craZ JeBCX2UmHwpAvMQmz3fVJJC0x+9+YptgLQEU6//KK/dBOPzLfOaqnSx9GoFTazcEyIrs ZeJV6/yRQf8q8IPdxFgBpwqfWeabgPDfjL4Rl/jKboGhUkKaiyLwFY5FhZwiZifKzTNR tidA== X-Gm-Message-State: AJcUukcVKuGIP2xoWf/Kw7dORC+06eVJjIQBhKuP0md6jvr8iD3e0fOO Au/vdqawp+o3khOG/lk9Vyszvjzy X-Google-Smtp-Source: ALg8bN7QwJ8VAaBMLQSICO26U0RU6cLj26bmEJ78QW6K0FsnvJUZ1nydLpCDinHc33dkus7HiuEdaw== X-Received: by 2002:a1c:35ca:: with SMTP id c193mr27795477wma.146.1548918556948; Wed, 30 Jan 2019 23:09:16 -0800 (PST) Received: from [88.208.79.100] (halouny.humusoft.cz. [88.208.79.100]) by smtp.gmail.com with ESMTPSA id v132sm4431719wme.20.2019.01.30.23.09.16 (version=TLS1_2 cipher=ECDHE-RSA-AES128-GCM-SHA256 bits=128/128); Wed, 30 Jan 2019 23:09:16 -0800 (PST) Sender: Michal Meloun From: Michal Meloun X-Google-Original-From: Michal Meloun Reply-To: mmel@freebsd.org Subject: Re: Auto expanding filesystem To: Russell Haley , freebsd-arm References: Openpgp: preference=signencrypt Autocrypt: addr=mmel@freebsd.org; prefer-encrypt=mutual; keydata= mQENBFYuVRkBCADZiwLCCne3wG9b9k+R2Neo5zVo2bLaZRfNNY/v9kg283i0sb1Da4EdEiNT 15El5UyozhphUIbIR/zrVpxF1TvvFdoCyzx6a68bNY2d9dBrDcNDZC+XnyDdHQoobN87DWT1 mRVkmbg9LHZ/SVUOkGYuWyE+8UYeDAcUizuXwSK5zFWmeTyIoWNa68ifrWLfQe0p4x5jC/AI VURCi17p360vU4fhgwoMvEEhrRBWCr4DYHToFjIt2WdBy3GR1qoO0+Xkd6G+OoBULo+XDfgu L2WdPvh0K69F9/LgHkMmG5Il7SCe62QGpG2vaCgRV7BQhLX+kxlvM+WrdRatWRml4Y/3ABEB AAG0IE1pY2hhbCBNZWxvdW4gPG1tZWxAZnJlZWJzZC5vcmc+iQFXBBMBCgBBAhsDBQsJCAcD BRUKCQgLBRYDAgEAAh4BAheAAhkBFiEEAN1KEEuAn+Apg413aR6ya17FqqoFAlw3aO8FCQ9v FVYACgkQaR6ya17FqqrIFwf/V/NRuAutw1cZ/HRCwfp00KY+8g730KwOaAMhPYvq8tqf8krD whFRWt9s4DSVTVJUC2dRZa5g1MS77iQL/WWzBUhJj7rW4uMpcKpi7UXi060sKrnE+1ZBvanG 8YCMTHKxQgQDD0cBqsyOAfrSA+Pyya3/HyAh1vvjQZfu5vWxA1X5NX5l5KtonprJ+ybVacwO W34yfWSX+ncx089JpUknenGdI+gVoKfa6uh/8YiCZTI5poxBttrOB8NGfylTsTTTbw2pkire Vkc87qq++I9bBNtTqWOZjB/3KBUd4q1veEUa4MS63TWtAvcEcsxHiBv4AH6npPO/iPycuGGh qldT1LkBDQRWLlUZAQgAuqBGR9LbUP86pYT2Zd+HZsiOun24LxPQwK6KZuysB0so02isa7ac T6t5uBfyfmdgzfvsc6dqU8bI65e8JtDwwVVF1Y4fF6cmNcmJqU10Gw5/bAu9re9JJWx2g/OJ tYMhwmqEE5DcS6GwgvJZI+9hgoSLL3mZ+GsO25NM4BhVH1o1AE4Q3O0HZMMnIzH+pma0augZ Xc3Qep17/Occ+1A7xEbn8VAYx8cwjkYUy7JyvVx4ecuj+i+uoCXhNhX5QdIcn4UMT1233Bcd yVZtZsLTI26ByFmrquGjkmN+/hra/s+nKfcegOKeHWVY/uFgDRk0TEYd6QuddZWo7+XMZLps wQARAQABiQElBBgBCgAPAhsMBQJZjBHDBQkHICOqAAoJEGkesmtexaqquysH/iDgRIrlMvFT GLyktZws/K/C03gWZ/tWwJV5+SFqRoasM+Z+9+cb44XA3rReqieLsYF5qSXTXHBPhEg1+9V9 KEPLpwektLtAv8zynN+6VVffwyRWQ4PIZmHCMT6PJP+Rk0DU6VrDc3ch58erduuyRDsbh32g 96nYMNvDsLhDvq44GPHLfglUHRY6wHo3IxAH2HosaWNC10R13JSrCdFnPMeIa+nSE+11hAdB mWpuPgVX2VNErtrwSBr7LsyCZ4yLO0bN5fKM0/Tavc9EcI9qDBrnts/EfZoCHhDtTMEFnQZM ybsMso20I/nxYPFuWuuFn7uQeoYrwWxt15SkN0RgtV2JATwEGAEKACYCGwwWIQQA3UoQS4Cf 4CmDjXdpHrJrXsWqqgUCXDdpmwUJD28WAgAKCRBpHrJrXsWqqtOrB/9Okk/dm2/mAs3tbA6l lKOZAwfUwBonwG7YhK9dOb5No/bJoY8G9s2IVXqwWKqCDv1qKC4M8pMXPD9fVsfNPG8GA1GZ rpZoZxHFteXZHoE1grpWypE0T3hp1W0hQNWXKv0MSuEMRVKU1m/iyLa10X7q8BaKtEDs35Xf DCh7eVg1vqiKtWyFn1u+y9Gy1Ztc/SKTs8mQvMYNUdBZuV6vN0VSz3I6wD9HVfo6Eo3M7cVp qqQ+KhrrGiCCYQPfZwpFAJSSgV3bR5O0BlNaGKJOoVTV1yexRbVEStswiFP8JFQp6U+S3nqE FFob7daQBLxi80oUVRn6eEdzR8tBhIy7sbeD Message-ID: <3e2e0631-166b-d74f-55a4-7bd6cb8464c3@freebsd.org> Date: Thu, 31 Jan 2019 08:09:18 +0100 User-Agent: Mozilla/5.0 (Windows NT 10.0; WOW64; rv:60.0) Gecko/20100101 Thunderbird/60.4.0 MIME-Version: 1.0 In-Reply-To: Content-Type: text/plain; charset=utf-8 Content-Language: en-US Content-Transfer-Encoding: 7bit X-Rspamd-Queue-Id: 57ED0741D3 X-Spamd-Bar: ------ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=gmail.com header.s=20161025 header.b=jEZ8CcRU; dmarc=pass (policy=none) header.from=gmail.com; spf=pass (mx1.freebsd.org: domain of melounmichal@gmail.com designates 2a00:1450:4864:20::335 as permitted sender) smtp.mailfrom=melounmichal@gmail.com X-Spamd-Result: default: False [-6.69 / 15.00]; RCVD_VIA_SMTP_AUTH(0.00)[]; HAS_REPLYTO(0.00)[mmel@freebsd.org]; FREEMAIL_FROM(0.00)[gmail.com]; R_SPF_ALLOW(-0.20)[+ip6:2a00:1450:4000::/36]; RCVD_COUNT_THREE(0.00)[3]; TO_DN_ALL(0.00)[]; DKIM_TRACE(0.00)[gmail.com:+]; RCPT_COUNT_TWO(0.00)[2]; DMARC_POLICY_ALLOW(-0.50)[gmail.com,none]; MX_GOOD(-0.01)[cached: alt3.gmail-smtp-in.l.google.com]; FREEMAIL_TO(0.00)[gmail.com]; FROM_EQ_ENVFROM(0.00)[]; RCVD_TLS_LAST(0.00)[]; MIME_TRACE(0.00)[0:+]; FREEMAIL_ENVFROM(0.00)[gmail.com]; ASN(0.00)[asn:15169, ipnet:2a00:1450::/32, country:US]; TAGGED_FROM(0.00)[]; DWL_DNSWL_NONE(0.00)[gmail.com.dwl.dnswl.org : 127.0.5.0]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; R_DKIM_ALLOW(-0.20)[gmail.com:s=20161025]; FROM_HAS_DN(0.00)[]; NEURAL_HAM_SHORT(-0.97)[-0.972,0]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; TAGGED_RCPT(0.00)[]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; REPLYTO_DOM_NEQ_FROM_DOM(0.00)[]; MIME_GOOD(-0.10)[text/plain]; TO_MATCH_ENVRCPT_SOME(0.00)[]; RCVD_IN_DNSWL_NONE(0.00)[5.3.3.0.0.0.0.0.0.0.0.0.0.0.0.0.0.2.0.0.4.6.8.4.0.5.4.1.0.0.a.2.list.dnswl.org : 127.0.5.0]; IP_SCORE(-2.71)[ip: (-9.23), ipnet: 2a00:1450::/32(-2.29), asn: 15169(-1.96), country: US(-0.07)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 07:09:20 -0000 On 30.01.2019 23:06, Russell Haley wrote: > Hi, > > I was wondering how the auto-expanding filesystem on the FreeBSD provided > arm images works? An RTFM link or link to code would be great. I just a > thread to pull on as I don't even know where to start. Is growfs(8) and https://svnweb.freebsd.org/base/head/libexec/rc/rc.d/growfs?view=log enough for start digging? Michal From owner-freebsd-arm@freebsd.org Thu Jan 31 08:30:11 2019 Return-Path: Delivered-To: freebsd-arm@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 E6807134D7E4 for ; Thu, 31 Jan 2019 08:30:10 +0000 (UTC) (envelope-from 5c52adf1747a448f399216cf-freebsd+2Darm=freebsd.org@return.mxmail.io) Received: from relay-7.emailamp.com (relay-7.emailamp.com [185.175.163.10]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id D28587763B for ; Thu, 31 Jan 2019 08:30:09 +0000 (UTC) (envelope-from 5c52adf1747a448f399216cf-freebsd+2Darm=freebsd.org@return.mxmail.io) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe; bh=+IH2c7G1608/qyrjKRQmsroHrzFLGSHh/rt+uCQ/oOw=; b=kE6uvoGXIMhzA8kX/jqQf9HBwS0EkdfQhryb4HJPSGlwiHNro0MOAf8muj0+yo12CHdFxrthwycS LckFOFPIw2JL7sCtix7LrGgqcYRMmL96XYWvwlg2agscr0H1IMyuHaYYqq/Ug2C3dGaNcFXd+9WR 39J0njJhlOgBpXjpF/IHnlLazalqXy0Uv+JMurw9TMqsPkzd1lD0qK59DsH2v6djFepNuQLBczLX TcImffs4b6z/T+dpsZ6LxD8yn/4M+vc3bP6QIycIJjI5l3OCxLw+meUQpIK2GjBkzdUkFBezos5/ 3kQNO10JnLxDrpTz/Yh67ZvLzutOffbr9XeJ3w== DKIM-Signature: v=1; a=rsa-sha256; c=simple; s=email; d=emailamp.com; h=Date:Subject:To:From:Reply-To:Content-Type:Message-Id:MIME-Version:List-Id: List-Unsubscribe:From:To:Subject; t=1548923409; x=1548945009; bh=HmvGZf+TfiQGETNMbJV+/aXcl55Ic+yhkcS/0TbFrR4=; b=D3EXLzmNaBDhG5bv+oRWF9vqfUJH0TSXygHsTbUI7+CSpKgZBCKz2Rz7zhYUNI9q+Wh9JvD+kiQU +pqaWXyxE2Eb8jpX/hrttNxtIeByOEVtQeEdMORVeBnHjByOQqsYUu2T31TB70sm4moTckfSggk3 CWBdmDobko/n/FnKcCym3/vT7hT2I7m0diaOkCI9JeKbUAv+28G9Zv2HlL+a3jv1162ghLl7z4YF C4PvA8RzhZBlPNPHCFdFlBP3n3+8qwoJHKZc0PK9fZJMZrhhi4VtQwgjQHB1RZ/mgZKD67hZ8t+U rYA0GN2njC+vhpQjj/4tUvlXYh8ObF/9wiEzww== Received: by mx-out-gi2.emailamp.com id haap122em8cl for ; Thu, 31 Jan 2019 03:23:54 -0500 (envelope-from <5c52adf1747a448f399216cf-freebsd+2Darm=freebsd.org@return.mxmail.io>) Date: Thu, 31 Jan 2019 10:23:54 +0200 Subject: An awe-inspiring address with world class facilities To: freebsd-arm@freebsd.org From: "MRAE Digital" Reply-To: Message-Id: List-Unsubscribe-Post: List-Unsubscribe=One-Click Bounces-to: 5c52adf1747a448f399216cf@return.mxmail.io X-Auto-Response-Suppress: All Original-from: reply@propinvestors.club Precedence: Bulk X-SES-CONFIGURATION-SET: mxm X-Rspamd-Queue-Id: D28587763B X-Spamd-Bar: ++++++ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=emailamp.com header.s=email header.b=kE6uvoGX; dkim=pass header.d=emailamp.com header.s=email header.b=D3EXLzmN; dmarc=fail reason="" header.from=propinvestors.club (policy=none) X-Spamd-Result: default: False [6.87 / 15.00]; HAS_REPLYTO(0.00)[reply@propinvestors.club]; TO_DN_NONE(0.00)[]; REPLYTO_ADDR_EQ_FROM(0.00)[]; DKIM_TRACE(0.00)[emailamp.com:+]; MX_GOOD(-0.01)[cached: return.mxmail.io]; FORGED_SENDER(0.30)[reply@propinvestors.club,5c52adf1747a448f399216cf-freebsd@return.mxmail.io]; RCVD_TLS_LAST(0.00)[]; IP_SCORE(0.60)[ip: (0.75), ipnet: 185.175.160.0/22(0.54), asn: 9009(1.81), country: GB(-0.09)]; ASN(0.00)[asn:9009, ipnet:185.175.160.0/22, country:GB]; MID_RHS_MATCH_FROM(0.00)[]; TAGGED_FROM(0.00)[2Darm=freebsd.org]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[emailamp.com:s=email]; FROM_NEQ_ENVFROM(0.00)[reply@propinvestors.club,5c52adf1747a448f399216cf-freebsd@return.mxmail.io]; FROM_HAS_DN(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; PRECEDENCE_BULK(0.00)[]; R_BAD_CTE_7BIT(1.05)[7bit,utf8]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; HAS_LIST_UNSUB(-0.01)[]; RCPT_COUNT_ONE(0.00)[1]; MANY_INVISIBLE_PARTS(1.00)[10]; NEURAL_SPAM_SHORT(0.84)[0.843,0]; NEURAL_SPAM_MEDIUM(1.00)[1.000,0]; HTML_SHORT_LINK_IMG_2(1.00)[]; NEURAL_SPAM_LONG(1.00)[1.000,0]; MIME_HTML_ONLY(0.20)[]; R_SPF_NA(0.00)[]; RCVD_COUNT_TWO(0.00)[2]; GREYLIST(0.00)[pass,body]; DMARC_POLICY_SOFTFAIL(0.10)[propinvestors.club : No valid SPF, DKIM not aligned (relaxed), none] X-Spam: Yes MIME-Version: 1.0 Content-Type: text/plain; charset="utf-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 08:30:11 -0000 From owner-freebsd-arm@freebsd.org Thu Jan 31 08:42:18 2019 Return-Path: Delivered-To: freebsd-arm@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 8C131134E36F for ; Thu, 31 Jan 2019 08:42:18 +0000 (UTC) (envelope-from freebsd-rwg@pdx.rh.CN85.dnsmgr.net) Received: from pdx.rh.CN85.dnsmgr.net (br1.CN84in.dnsmgr.net [69.59.192.140]) (using TLSv1 with cipher DHE-RSA-AES256-SHA (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id D3D5780068 for ; Thu, 31 Jan 2019 08:42:17 +0000 (UTC) (envelope-from freebsd-rwg@pdx.rh.CN85.dnsmgr.net) Received: from pdx.rh.CN85.dnsmgr.net (localhost [127.0.0.1]) by pdx.rh.CN85.dnsmgr.net (8.13.3/8.13.3) with ESMTP id x0V8g8Se017051; Thu, 31 Jan 2019 00:42:08 -0800 (PST) (envelope-from freebsd-rwg@pdx.rh.CN85.dnsmgr.net) Received: (from freebsd-rwg@localhost) by pdx.rh.CN85.dnsmgr.net (8.13.3/8.13.3/Submit) id x0V8g7CA017050; Thu, 31 Jan 2019 00:42:07 -0800 (PST) (envelope-from freebsd-rwg) From: "Rodney W. Grimes" Message-Id: <201901310842.x0V8g7CA017050@pdx.rh.CN85.dnsmgr.net> Subject: Re: Auto expanding filesystem In-Reply-To: To: Russell Haley Date: Thu, 31 Jan 2019 00:42:07 -0800 (PST) CC: freebsd-arm X-Mailer: ELM [version 2.4ME+ PL121h (25)] MIME-Version: 1.0 Content-Transfer-Encoding: 7bit Content-Type: text/plain; charset=US-ASCII X-Rspamd-Queue-Id: D3D5780068 X-Spamd-Bar: + Authentication-Results: mx1.freebsd.org X-Spamd-Result: default: False [1.16 / 15.00]; ARC_NA(0.00)[]; FROM_HAS_DN(0.00)[]; IP_SCORE(-0.01)[ip: (0.02), ipnet: 69.59.192.0/19(0.01), asn: 13868(-0.02), country: US(-0.07)]; TAGGED_RCPT(0.00)[]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[dnsmgr.net]; AUTH_NA(1.00)[]; NEURAL_SPAM_MEDIUM(0.56)[0.561,0]; NEURAL_HAM_LONG(-0.26)[-0.258,0]; RCVD_COUNT_THREE(0.00)[3]; TO_MATCH_ENVRCPT_SOME(0.00)[]; TO_DN_ALL(0.00)[]; MX_GOOD(-0.01)[cached: pdx.rh.CN85.dnsmgr.net]; RCPT_COUNT_TWO(0.00)[2]; NEURAL_HAM_SHORT(-0.02)[-0.022,0]; R_SPF_NA(0.00)[]; FREEMAIL_TO(0.00)[gmail.com]; FROM_EQ_ENVFROM(0.00)[]; R_DKIM_NA(0.00)[]; MIME_TRACE(0.00)[0:+]; ASN(0.00)[asn:13868, ipnet:69.59.192.0/19, country:US]; MID_RHS_MATCH_FROM(0.00)[]; RCVD_TLS_LAST(0.00)[] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 08:42:18 -0000 > Hi, > > I was wondering how the auto-expanding filesystem on the FreeBSD provided > arm images works? An RTFM link or link to code would be great. I just a > thread to pull on as I don't even know where to start. growfs(8) man growfs -- Rod Grimes rgrimes@freebsd.org From owner-freebsd-arm@freebsd.org Thu Jan 31 08:03:59 2019 Return-Path: Delivered-To: freebsd-arm@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 45CFA134C277 for ; Thu, 31 Jan 2019 08:03:59 +0000 (UTC) (envelope-from mad@madpilot.net) Received: from mail.madpilot.net (vogon.madpilot.net [159.69.1.99]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id A6F887677C for ; Thu, 31 Jan 2019 08:03:56 +0000 (UTC) (envelope-from mad@madpilot.net) Received: from mail (mail [192.168.254.3]) by mail.madpilot.net (Postfix) with ESMTP id 43qt6F1NdLz6dP7; Thu, 31 Jan 2019 09:03:49 +0100 (CET) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=madpilot.net; h= content-transfer-encoding:content-language:content-type :content-type:in-reply-to:mime-version:user-agent:date:date :message-id:from:from:references:subject:subject:received :received; s=mail; t=1548921823; x=1550736224; bh=zkJ1dAdyZHyy5Q 7zxjjPTFLB9Dd3RGcDcizj2jmQHFY=; b=FkoVO9LV+FITybyqKE6Pc5XGOfEdSM EPynh+R2HshbDzzUjMrhOE8bVBcF96n5Emsyu0x8WH5IzhSO89fyJZSMlO6nVSas 8QFz1Tvns+mlRXWXQwmm4I23MldKXlzMjCEhcNptOXgWVZrI2BOnpqUUG+WTJHAt zYATK3x9DfY9c= Received: from mail.madpilot.net ([192.168.254.3]) by mail (mail.madpilot.net [192.168.254.3]) (amavisd-new, port 10026) with ESMTP id D4rGjAVDHvtT; Thu, 31 Jan 2019 09:03:43 +0100 (CET) Received: from marvin.madpilot.net (unknown [87.13.153.156]) (using TLSv1.3 with cipher TLS_AES_128_GCM_SHA256 (128/128 bits) key-exchange X25519 server-signature RSA-PSS (2048 bits) server-digest SHA256) (No client certificate requested) by mail.madpilot.net (Postfix) with ESMTPSA; Thu, 31 Jan 2019 09:03:43 +0100 (CET) Subject: Re: Auto expanding filesystem To: Russell Haley , freebsd-arm References: From: Guido Falsi Openpgp: preference=signencrypt Autocrypt: addr=mad@madpilot.net; prefer-encrypt=mutual; keydata= mQENBE+G+l0BCADi/WBQ0aRJfnE7LBPsM0G3m/m3Yx7OPu4iYFvS84xawmRHtCNjWIntsxuX fptkmEo3Rsw816WUrek8dxoUAYdHd+EcpBcnnDzfDH5LW/TZ4gbrFezrHPdRp7wdxi23GN80 qPwHEwXuF0X4Wy5V0OO8B6VT/nA0ADYnBDhXS52HGIJ/GCUjgqJn+phDTdCFLvrSFdmgx4Wl c0W5Z1p5cmDF9l8L/hc959AeyNf7I9dXnjekGM9gVv7UDUYzCifR3U8T0fnfdMmS8NeI9NC+ wuREpRO4lKOkTnj9TtQJRiptlhcHQiAlG1cFqs7EQo57Tqq6cxD1FycZJLuC32bGbgalABEB AAG0Hkd1aWRvIEZhbHNpIDxtYWRAbWFkcGlsb3QubmV0PokBOQQTAQgAIwIbAwIeAQIXgAUL CQgHAwUVCgkICwQWAgMBBQJS79AgAhkBAAoJEBrmhg5Wy9KTc0kH/RO64ORBlTbTHaUaOj8F Je5O5NU2Pt9Cyt5ZWBRvxntr1zPTJGKRPS9ihlIfqT4ZvEngQGp57EUyFbCpI0UWasTerImM tt5WACnGmCzUTB39UXx8Oy4b1EgWeTJQ747e/F1mQLXTNa6ijRBE9fYlTb4gAkPN88/wVV9v 3PZozKLTg16ghBzHM/P7Lk8L7clPEZChX1FTa/6eSt3nvzfCuTMZbBPJF/ph+q1KyPqRgVfh tyhu5dvgMoPz/ni41IfeSrkJTD5RXzdyGR9q4Z1NYeBsLkRjC4LxKAP5KqUsvlOUjKvO1byj ApYdMarol+IGkaSk9e3zVYAJkWKjn/ni8Xa5Ag0EUxB7QQEQAKFhrDceoPdK/IHDSmoj6SQY isvM7VdhcleS7E9DoEAVt7yMbf6HbbMVTTY6ckvwTWQssywLBXNVqxgc4WLJjzfUhgef+WE7 5M3+WFYlOVQLGZY/zEVgma1raYnOHNAOzeHLDmEXjbZP6vGAeDyBbGfQPpE7qGYZ7ubeT3Xw QO+PklcCrvOPj2ZPcAxGNS2xVU/LzONqCrJqLMJSIcCdsbiSP4G5PnDFHtMokaTY6OEr8OEQ fOAerhcHUa/z7Uu8YtmaqKH+QGkE/WEgaRqSiTnv0JOTD+DxehaqvoKPPZ++2NpCZMHB2i6A /xifmQwEiIjEXtcueBRzkNUQkxhqZyS13SrhocL9ydtaVPBzZatAEjUDDEJmAMLVFs45qfyh MiNapHJo2n3MW/E5omqCvEkDdWX/en3P7CK2TemeaDghMsgkNKax/z0wNo5UZCkOPOz0xpNi UilOVbkuezZZNg65741qee2lfXhQIaZ66yT7hphc/N/z3PIAtLeze4u1VR2EXAuZ2sWAdlKC NTlJMsaU/x70BV11Wd/ypnVzM68dfdQIIAj1iMFAD/lXGlEUmKXg5Ov2VQDlTntQoanCYrAg +8CttPzjrydgLZFq3hrtQmfc0se5yv1WHS69+BsUOG09RvvawUDZxUjW19kyeN9THaNRgow3 kSuArUp6zSmJABEBAAGJAR8EGAEIAAkFAlMQe0ECGwwACgkQGuaGDlbL0pMN5wgA4bCkX/qw EVC06ToeR6C2putmSWQMgpDaqrv65Hubo+QGmg2P4ewTYQQ4g6oYWS03qHxqVVWhKz7FjfrV +dH8qbCLfSgIcvdBha7ayGZVrsiuMLKGbw36fcmkZPpSDOfHcP0XH8Z+u9CWj0xUkTxAlZ/7 i6gYSUpG2JWNtdmE/X8VVEyXusCLwy0K0BI60A/4dRTIX3C4QKrJ3ZbUXegz70ynjHf+lQMZ 9IZKASoRMuS5FozPQh6abvmwZEPdf5I9riUElzvHrqJ8Bx0t3Pujdoth+yNHpnBxrtO8LkQd rQ58P0SwcaIX33T2U9pG8bhu5YVR88FQ8OQ0cEsPBpDncg== Message-ID: Date: Thu, 31 Jan 2019 09:03:42 +0100 User-Agent: Mozilla/5.0 (X11; FreeBSD amd64; rv:60.0) Gecko/20100101 Thunderbird/60.5.0 MIME-Version: 1.0 In-Reply-To: Content-Type: text/plain; charset=utf-8 Content-Language: en-US Content-Transfer-Encoding: 7bit X-Rspamd-Queue-Id: A6F887677C X-Spamd-Bar: ------ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=madpilot.net header.s=mail header.b=FkoVO9LV; spf=pass (mx1.freebsd.org: domain of mad@madpilot.net designates 159.69.1.99 as permitted sender) smtp.mailfrom=mad@madpilot.net X-Spamd-Result: default: False [-6.21 / 15.00]; ARC_NA(0.00)[]; RCVD_VIA_SMTP_AUTH(0.00)[]; R_DKIM_ALLOW(-0.20)[madpilot.net:s=mail]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; FROM_HAS_DN(0.00)[]; R_SPF_ALLOW(-0.20)[+mx]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; TAGGED_RCPT(0.00)[]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[madpilot.net]; NEURAL_HAM_SHORT(-0.94)[-0.939,0]; RCVD_COUNT_THREE(0.00)[4]; TO_MATCH_ENVRCPT_SOME(0.00)[]; TO_DN_ALL(0.00)[]; DKIM_TRACE(0.00)[madpilot.net:+]; RCPT_COUNT_TWO(0.00)[2]; MX_GOOD(-0.01)[eddie.gfratio.it,vogon.madpilot.net]; RCVD_TLS_LAST(0.00)[]; FREEMAIL_TO(0.00)[gmail.com]; RECEIVED_SPAMHAUS_PBL(0.00)[156.153.13.87.zen.spamhaus.org : 127.0.0.10]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; ASN(0.00)[asn:24940, ipnet:159.69.0.0/16, country:DE]; MID_RHS_MATCH_FROM(0.00)[]; IP_SCORE(-2.76)[ip: (-9.62), ipnet: 159.69.0.0/16(-1.93), asn: 24940(-2.26), country: DE(-0.01)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 08:03:59 -0000 On 30/01/19 23:06, Russell Haley wrote: > Hi, > > I was wondering how the auto-expanding filesystem on the FreeBSD provided > arm images works? An RTFM link or link to code would be great. I just a > thread to pull on as I don't even know where to start. Did not check how the images are structured, but there's /etc/rc.d/growfs which looks like what you're searching for. -- Guido Falsi From owner-freebsd-arm@freebsd.org Thu Jan 31 07:14:18 2019 Return-Path: Delivered-To: freebsd-arm@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 63C5513492BD for ; Thu, 31 Jan 2019 07:14:18 +0000 (UTC) (envelope-from lwhsu.freebsd@gmail.com) Received: from mail-yw1-f46.google.com (mail-yw1-f46.google.com [209.85.161.46]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "smtp.gmail.com", Issuer "Google Internet Authority G3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 8E62074557 for ; Thu, 31 Jan 2019 07:14:17 +0000 (UTC) (envelope-from lwhsu.freebsd@gmail.com) Received: by mail-yw1-f46.google.com with SMTP id j82so905169ywb.2 for ; Wed, 30 Jan 2019 23:14:17 -0800 (PST) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:mime-version:references:in-reply-to:from:date :message-id:subject:to:cc; bh=8Z69Kycc5igFNV55E1BfJyKOzZNUUktmxIJSqAB0aEk=; b=bk1ibaE3TPxznUcFQuEVy0aXHhPXtbGEHtMS+bmhVuZ14eUzqOVZL+fU0kzJUMzcLg 6zGmN1ETsTs7d2qWABKSrNO0IRDDnDHnzZ70EKsLJ0y/qvtn3Gpc/iAi8gTG5ypB/cq2 ccg6vXiRr7nS6Kea+tzkkmjHpaZWr0PsouuPtlXqqm9H3ZzZ2Snx6edNU2j0H/FGazp6 1FbuX0P29hZriN5tQ9Uj7fddIgzCYbtmLoZ5M5mXHToI8cVFf2+Ej/bxqLR7X8P9srrG W7Dda9yL8H9khJ5T6paiog+cL9t1nUmnaLNYRNSKTdJwJoJK0F1JrZffionIBp8awQ0G xA/A== X-Gm-Message-State: AJcUukcSBLpN/vIQALMmhbpw6UhJ3VyPxmOPcI0bkvRygUgnlG4NmrhZ B5HkMJvl8gA9tQLXbmmMs6YnhBJy6AEaNh6LOBA= X-Google-Smtp-Source: ALg8bN4HAB1iRif8gF7lI2ZekblQb8hgFyFTejRF1XWoLMaTlH6OS0UYmnoFWPPzugsp+0jJwd7IsOXl/9opSqTmUPg= X-Received: by 2002:a81:2714:: with SMTP id n20mr32038010ywn.77.1548918855831; Wed, 30 Jan 2019 23:14:15 -0800 (PST) MIME-Version: 1.0 References: In-Reply-To: From: Li-Wen Hsu Date: Thu, 31 Jan 2019 15:14:04 +0800 Message-ID: Subject: Re: Auto expanding filesystem To: Russell Haley Cc: freebsd-arm Content-Type: text/plain; charset="UTF-8" X-Rspamd-Queue-Id: 8E62074557 X-Spamd-Bar: --- Authentication-Results: mx1.freebsd.org; spf=pass (mx1.freebsd.org: domain of lwhsufreebsd@gmail.com designates 209.85.161.46 as permitted sender) smtp.mailfrom=lwhsufreebsd@gmail.com X-Spamd-Result: default: False [-3.32 / 15.00]; R_SPF_ALLOW(-0.20)[+ip4:209.85.128.0/17]; TO_DN_ALL(0.00)[]; MX_GOOD(-0.01)[cached: alt3.gmail-smtp-in.l.google.com]; RCPT_COUNT_TWO(0.00)[2]; NEURAL_HAM_SHORT(-0.16)[-0.161,0]; FORGED_SENDER(0.30)[lwhsu@freebsd.org,lwhsufreebsd@gmail.com]; FREEMAIL_TO(0.00)[gmail.com]; IP_SCORE(-1.15)[ipnet: 209.85.128.0/17(-3.73), asn: 15169(-1.96), country: US(-0.07)]; R_DKIM_NA(0.00)[]; FREEMAIL_ENVFROM(0.00)[gmail.com]; ASN(0.00)[asn:15169, ipnet:209.85.128.0/17, country:US]; TAGGED_FROM(0.00)[]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; FROM_NEQ_ENVFROM(0.00)[lwhsu@freebsd.org,lwhsufreebsd@gmail.com]; FROM_HAS_DN(0.00)[]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; TAGGED_RCPT(0.00)[]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; DMARC_NA(0.00)[freebsd.org]; MIME_GOOD(-0.10)[text/plain]; MIME_TRACE(0.00)[0:+]; TO_MATCH_ENVRCPT_SOME(0.00)[]; RCVD_IN_DNSWL_NONE(0.00)[46.161.85.209.list.dnswl.org : 127.0.5.0]; RCVD_TLS_LAST(0.00)[]; RCVD_COUNT_TWO(0.00)[2] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 07:14:18 -0000 On Thu, Jan 31, 2019 at 2:27 PM Russell Haley wrote: > > Hi, > > I was wondering how the auto-expanding filesystem on the FreeBSD provided > arm images works? An RTFM link or link to code would be great. I just a > thread to pull on as I don't even know where to start. Please see release/tools/arm.subr, there are growfs_enable="YES" and touch /firstboot From owner-freebsd-arm@freebsd.org Thu Jan 31 07:31:29 2019 Return-Path: Delivered-To: freebsd-arm@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 0EEF6134A2A5 for ; Thu, 31 Jan 2019 07:31:29 +0000 (UTC) (envelope-from darius@dons.net.au) Received: from ipmail07.adl2.internode.on.net (ipmail07.adl2.internode.on.net [150.101.137.131]) by mx1.freebsd.org (Postfix) with ESMTP id 5AB6C74FB3 for ; Thu, 31 Jan 2019 07:31:20 +0000 (UTC) (envelope-from darius@dons.net.au) Received: from ppp118-210-70-131.bras2.adl4.internode.on.net (HELO midget.dons.net.au) ([118.210.70.131]) by ipmail07.adl2.internode.on.net with ESMTP; 31 Jan 2019 18:01:10 +1030 Received: from midget.dons.net.au (localhost [127.0.0.1]) by midget.dons.net.au (8.15.2/8.15.2) with ESMTPS id x0V7UokI092094 (version=TLSv1.2 cipher=ECDHE-RSA-AES256-GCM-SHA384 bits=256 verify=NO) for ; Thu, 31 Jan 2019 18:01:05 +1030 (ACDT) (envelope-from darius@dons.net.au) Received: (from mailnull@localhost) by midget.dons.net.au (8.15.2/8.15.2/Submit) id x0V77TWm074884 for ; Thu, 31 Jan 2019 17:37:29 +1030 (ACDT) (envelope-from darius@dons.net.au) X-Authentication-Warning: midget.dons.net.au: mailnull set sender to using -f Received: from [203.31.81.59] ([203.31.81.59]) by ppp118-210-70-131.bras2.adl4.internode.on.net (envelope-sender ) (MIMEDefang) with ESMTP id x0V77OTD074882; Thu, 31 Jan 2019 17:37:29 +1030 Content-Type: text/plain; charset=us-ascii Mime-Version: 1.0 (Mac OS X Mail 12.2 \(3445.102.3\)) Subject: Re: Auto expanding filesystem From: "O'Connor, Daniel" In-Reply-To: Date: Thu, 31 Jan 2019 17:37:56 +1030 Cc: freebsd-arm Content-Transfer-Encoding: quoted-printable Message-Id: <49828A1A-C4BE-4DD0-9DF8-63B99127E9BA@dons.net.au> References: To: Russell Haley X-Mailer: Apple Mail (2.3445.102.3) X-Spam-Score: 1.3 (*) No, score=1.3 required=5.0 tests=HELO_MISC_IP, RDNS_NONE autolearn=no autolearn_force=no version=3.4.1 X-Scanned-By: MIMEDefang 2.83 on 10.0.2.1 X-Rspamd-Queue-Id: 5AB6C74FB3 X-Spamd-Bar: ++++ Authentication-Results: mx1.freebsd.org X-Spamd-Result: default: False [4.16 / 15.00]; MV_CASE(0.50)[]; HAS_XAW(0.00)[]; TO_DN_ALL(0.00)[]; MX_GOOD(-0.01)[midget.dons.net.au]; RCPT_COUNT_TWO(0.00)[2]; FREEMAIL_TO(0.00)[gmail.com]; RCVD_NO_TLS_LAST(0.10)[]; RECEIVED_SPAMHAUS_PBL(0.00)[131.70.210.118.zen.spamhaus.org : 127.0.0.11]; IP_SCORE(0.40)[ipnet: 150.101.0.0/16(1.64), asn: 4739(0.42), country: AU(-0.04)]; R_DKIM_NA(0.00)[]; ASN(0.00)[asn:4739, ipnet:150.101.0.0/16, country:AU]; MIME_TRACE(0.00)[0:+]; MID_RHS_MATCH_FROM(0.00)[]; FROM_EQ_ENVFROM(0.00)[]; ARC_NA(0.00)[]; RCVD_COUNT_FIVE(0.00)[5]; RCVD_IN_DNSWL_LOW(-0.10)[131.137.101.150.list.dnswl.org : 127.0.5.1]; FROM_HAS_DN(0.00)[]; NEURAL_SPAM_SHORT(0.42)[0.418,0]; TAGGED_RCPT(0.00)[]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; DMARC_NA(0.00)[dons.net.au]; MIME_GOOD(-0.10)[text/plain]; NEURAL_SPAM_MEDIUM(0.97)[0.970,0]; AUTH_NA(1.00)[]; TO_MATCH_ENVRCPT_SOME(0.00)[]; NEURAL_SPAM_LONG(0.98)[0.978,0]; R_SPF_NA(0.00)[] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 07:31:29 -0000 > On 31 Jan 2019, at 08:36, Russell Haley wrote: > I was wondering how the auto-expanding filesystem on the FreeBSD = provided > arm images works? An RTFM link or link to code would be great. I just = a > thread to pull on as I don't even know where to start. They work by using gpart to resize then run growfs. = https://svnweb.freebsd.org/base/release/11.2.0/etc/rc.d/growfs?revision=3D= 335563&view=3Dmarkup (Not sure where it got moved in head..) -- Daniel O'Connor "The nice thing about standards is that there are so many of them to choose from." -- Andrew Tanenbaum From owner-freebsd-arm@freebsd.org Thu Jan 31 17:49:02 2019 Return-Path: Delivered-To: freebsd-arm@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 A7C0414B172E for ; Thu, 31 Jan 2019 17:49:02 +0000 (UTC) (envelope-from mw@semihalf.com) Received: from mail-qk1-x742.google.com (mail-qk1-x742.google.com [IPv6:2607:f8b0:4864:20::742]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "smtp.gmail.com", Issuer "Google Internet Authority G3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 22DEA6A298 for ; Thu, 31 Jan 2019 17:49:01 +0000 (UTC) (envelope-from mw@semihalf.com) Received: by mail-qk1-x742.google.com with SMTP id 68so2365039qke.9 for ; Thu, 31 Jan 2019 09:49:01 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=semihalf-com.20150623.gappssmtp.com; s=20150623; h=mime-version:references:in-reply-to:from:date:message-id:subject:to :cc:content-transfer-encoding; bh=dd5fDk+HX8U0r/pJ0oUqqDtuNKS17bOqEiKdLWfEEcA=; b=Zu6ijo6y7tSO/JAkUGzZcVJyY4K5j+e7OAxJUQLewkwsM9Q5wL6yjUZ1ki1y+ftwcl 45pTafuKUlxRqjzpNusrNa1CBm3ok9sMwlPURSZBtkNpku36m2Xm50z4MP0DzhCFR0XG KkEJ4KfqYBYNdKNtd1z0S4R3paLuZe26G8lw48t5s4N73CgwTCl0BLO/m/1qwtcgP0Q8 xgU5GtexXXFTqnc/qFrYq3EwCfh4zSxmSEsMHp2rpER3fqeKktR6tzF46Arv+0ZESFST viV+u7k21bSSai76JPiC+Yd11rSh1QD6drgTtc60uj0YYc88/iESOvaKWToAFdzN2+V7 GMvg== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:mime-version:references:in-reply-to:from:date :message-id:subject:to:cc:content-transfer-encoding; bh=dd5fDk+HX8U0r/pJ0oUqqDtuNKS17bOqEiKdLWfEEcA=; b=SAJNPLbPpSqfuhKGHzuv7pzf9bYv6+Fgbjp6s5I0pCOiYPqs8VqIFmf1QlLzj0vO8K xRpbNU3cWuyzJZ9d7F2RS7DaKojJlk4i9H2n81QUKwqZ0lcuYjLXj0/y1pLQKcT9MHGb GaPIPdzFSsyx7zRfMxQBkVDnnWoxAHk/86ztF4gsVLyvMZRlX4Z0ZAlxdQIEhNXXPGQC Yn7R12lpLWfT0D2Zw009wXuzfOoj7i0lv9dNBJziPw5d7ev8OTVCBghTc4bnh+bOqzp+ 5XmSn0NYLy3vqSuxSV6B43P6mHnhYU1pi/w0yo5ir+WXVRCy3xRIZ87thlg/nV4rw4FO 8byQ== X-Gm-Message-State: AJcUukeqfU6cdZYM5sK8Lp32M/jrMPr1q94BHgmO8JdgfFFUPh1Zd87X UI9gmXyYBEbNuYpYxKQQ7/IZA9BWEi0wvqTWAN5qGw== X-Google-Smtp-Source: ALg8bN5u3sIEVoeuVUQcGmdgOUD0bvbdsr5NjkJR/6fawspRVvJ5+B4ID1SWymEciecygOcicw2iZcRnWOgSjwy+gX4= X-Received: by 2002:a37:781:: with SMTP id 123mr32452266qkh.231.1548956940525; Thu, 31 Jan 2019 09:49:00 -0800 (PST) MIME-Version: 1.0 References: In-Reply-To: From: Marcin Wojtas Date: Thu, 31 Jan 2019 18:48:48 +0100 Message-ID: Subject: Re: Help getting Marvell-A388 SBC booted To: doc.solo@web.de Cc: freebsd-arm Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Rspamd-Queue-Id: 22DEA6A298 X-Spamd-Bar: - Authentication-Results: mx1.freebsd.org; dkim=pass header.d=semihalf-com.20150623.gappssmtp.com header.s=20150623 header.b=Zu6ijo6y X-Spamd-Result: default: False [-1.89 / 15.00]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-0.72)[-0.721,0]; R_DKIM_ALLOW(-0.20)[semihalf-com.20150623.gappssmtp.com:s=20150623]; FROM_HAS_DN(0.00)[]; TO_DN_SOME(0.00)[]; NEURAL_SPAM_SHORT(0.22)[0.225,0]; NEURAL_HAM_LONG(-0.96)[-0.963,0]; MIME_GOOD(-0.10)[text/plain]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; DMARC_NA(0.00)[semihalf.com]; TO_MATCH_ENVRCPT_SOME(0.00)[]; DKIM_TRACE(0.00)[semihalf-com.20150623.gappssmtp.com:+]; RCPT_COUNT_TWO(0.00)[2]; RCVD_IN_DNSWL_NONE(0.00)[2.4.7.0.0.0.0.0.0.0.0.0.0.0.0.0.0.2.0.0.4.6.8.4.0.b.8.f.7.0.6.2.list.dnswl.org : 127.0.5.0]; MX_GOOD(-0.01)[ASPMX2.GOOGLEMAIL.com,ALT2.ASPMX.L.GOOGLE.com,ASPMX.L.GOOGLE.com,ALT1.ASPMX.L.GOOGLE.com,ASPMX3.GOOGLEMAIL.com]; R_SPF_NA(0.00)[]; FREEMAIL_TO(0.00)[web.de]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_TLS_LAST(0.00)[]; ASN(0.00)[asn:15169, ipnet:2607:f8b0::/32, country:US]; RCVD_COUNT_TWO(0.00)[2]; IP_SCORE(-0.13)[ip: (3.97), ipnet: 2607:f8b0::/32(-2.55), asn: 15169(-1.97), country: US(-0.07)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 17:49:02 -0000 Hi S=C3=B6ren, =C5=9Br., 30 sty 2019 o 18:03 napisa=C5=82(a): > > Hi, > > I'm trying to get FreeBSD-12 booted on this device: https://wiki.kobol.io= / > > It's a Marvell-A388 based SBC. > > No matter what I tried, I got this output: > > --- > Autoboot in 0 seconds, hit [Enter] to boot or any other key to stop > > Loading kernel... > /boot/kernel/kernel text=3D0x864d6c data=3D0xb0da0+0x1f54e0 syms=3D[0x4+0= xa1060+0x4+0x101505] > Loading configured modules... > can't find '/boot/entropy' > Using DTB provided by U-Boot at address 0x2040000. > Kernel entry at 0x2400180... > Kernel args: (null) > --- > > No error message, nothing. I tried several U-Boot-versions, different par= ameters, loading addresses. The U-Boot part seems to work just fine. I thin= k its ubldr that doesn't get the kernel loaded properly. > I haven't launched it for a couple of months, but I'm not aware of any issue with HEAD on Armada38x. I'll try to check on one of my boards. > Do I need the FreeBSD specific U-Boot from ports? What makes them special= ? What does ubldr need to load the kernel? What should I try to debug any f= urther? Thanks for your help. > Which version of u-boot are you using? I guess it may be a device tree issue - is the one @0x2040000 basing on the sys/gnu/dts/arm/ version (equivalent of the mainline Linux kernel one)? Which config are you using? Best regards, Marcin > Regards, > > S=C3=B6ren > > _______________________________________________ > freebsd-arm@freebsd.org mailing list > https://lists.freebsd.org/mailman/listinfo/freebsd-arm > To unsubscribe, send any mail to "freebsd-arm-unsubscribe@freebsd.org" From owner-freebsd-arm@freebsd.org Thu Jan 31 22:23:40 2019 Return-Path: Delivered-To: freebsd-arm@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 C77AD14B9F5C for ; Thu, 31 Jan 2019 22:23:40 +0000 (UTC) (envelope-from doc.solo@web.de) Received: from mout.web.de (mout.web.de [212.227.17.12]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "mout.web.de", Issuer "TeleSec ServerPass DE-2" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id ACCD7759F1 for ; Thu, 31 Jan 2019 22:23:39 +0000 (UTC) (envelope-from doc.solo@web.de) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=web.de; s=dbaedf251592; t=1548973414; bh=jzL0bRkpq6oNjDGKTTwfoYDI2dukpcoWSg5ZbohS0DQ=; h=X-UI-Sender-Class:From:To:Subject:Date:In-Reply-To:References; b=PxLhMYPPkKBR01r9GDafTUtBDPWlkTdUFxxrihFs3VMaLt/eCxRQU9S62ZJWIsiDA qevZ1ofg1farrwWjJB2IH+iXZj9uUSEILvTw47qZ3zoPW2jZlokn2zUUtt2amz9uYn wx+lZC//VkYCL4CUs2qHoPT/oNJ3nH529soqhIpA= X-UI-Sender-Class: c548c8c5-30a9-4db5-a2e7-cb6cb037b8f9 Received: from [95.208.153.190] ([95.208.153.190]) by web-mail.web.de (3c-app-webde-bap37.server.lan [172.19.172.37]) (via HTTP); Thu, 31 Jan 2019 23:10:31 +0100 Message-ID: From: doc.solo@web.de To: freebsd-arm@freebsd.org Subject: Aw: Re: Help getting Marvell-A388 SBC booted Date: Thu, 31 Jan 2019 23:10:31 +0100 Importance: normal Sensitivity: Normal In-Reply-To: References: X-UI-Message-Type: mail X-Priority: 3 X-Provags-ID: V03:K1:SvIgrH+C0qWX24mMsnxRtoxDk99ZUpnobdoPfCirbtRISP58l7AME0Ae2BwRQ710oXQk/ /GBu4s9svUYZW0D9q1nsxLoFKgqoNBluOhytCSAu63bOIOYJCyfg8GFQFeVLjBZalebVlya6ybRk AvY46k423vDRcbWE1YJsUiWkQUTxWDpvWHQbba28b6NFMNqWVqXkChzh9S0sZdak6prG/xTkVc+X SzehWT3eSloZW/Wno8PBIUilSufPkTupM2z+moEQnQgMKTrLXNuEEQLGBotVbdL8TXVQ3Cb9EBTl JM= X-Spam-Flag: NO X-UI-Out-Filterresults: notjunk:1;V03:K0:a+s+fYUm9Ls=:DkvJxlerT8qt7/DT6FZF7z w83qeZ2Ij67W+WGjfj6iArC5W41CogAcglcaCw+cNYvjUQN/TVHmwVzUnLmt59uJ9/xgyGNt7 6dm6zV9O3DhgHvLCbQHLH1ELXTj6LkWpVgVUROF5m7+fiu04F3gXzg2IURh1kE/rhyWUb1hQN N3S2j4Xk6PBSghcJcF4EZyVh9Gc7kMNUK2KAVQKJ2uGqNyZO73hGhe8rIvkCB2Gt5YV8gMkbs /WU0dIarunTJ1ngcZ9OkNBxMsLRHEWuXg7mGu+vctpUmlWJSBj0DdE647ifc7j0dhArW1uIc1 LlsAmn0rXsd4AmOMdmi/LIZi+XsW08TVzXjZsFwIC4xJRd/Ab2vvP6P8HuOI2IHeBszvX0uP7 xbiBfJpoLOxxgC5oYQARVaa5s1YiiF1LOuEQe5t09uJKeXXVXtP9rjzgwdaw4dVfTFMj9PykO lvmbW7iylBOKeBkJTZmhypIugpoVeOfhXzPnVFGyyENih6zYwzNljyOogL9WdFciMFv5SsfXI HrcOrD9WOQmVoav4VXHQ2eAzDsekAJpzwLQxMHlT3Vijhn7vbOCc5DgSga5IYmYuHQJ3n4WBm xzTviIjL+qvd0= X-Rspamd-Queue-Id: ACCD7759F1 X-Spamd-Bar: / Authentication-Results: mx1.freebsd.org; dkim=pass header.d=web.de header.s=dbaedf251592 header.b=PxLhMYPP; spf=pass (mx1.freebsd.org: domain of doc.solo@web.de designates 212.227.17.12 as permitted sender) smtp.mailfrom=doc.solo@web.de X-Spamd-Result: default: False [0.90 / 15.00]; R_SPF_ALLOW(-0.20)[+ip4:212.227.17.0/27]; FREEMAIL_FROM(0.00)[web.de]; TO_DN_NONE(0.00)[]; DKIM_TRACE(0.00)[web.de:+]; MX_GOOD(-0.01)[mx-ha02.web.de,mx-ha03.web.de]; HAS_X_PRIO_THREE(0.00)[3]; RCVD_IN_DNSWL_LOW(-0.10)[12.17.227.212.list.dnswl.org : 127.0.5.1]; RECEIVED_SPAMHAUS_PBL(0.00)[190.153.208.95.zen.spamhaus.org : 127.0.0.10]; FREEMAIL_ENVFROM(0.00)[web.de]; ASN(0.00)[asn:8560, ipnet:212.227.0.0/16, country:DE]; RCVD_TLS_LAST(0.00)[]; FROM_EQ_ENVFROM(0.00)[]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[web.de:s=dbaedf251592]; IP_SCORE(0.27)[ipnet: 212.227.0.0/16(-0.75), asn: 8560(2.09), country: DE(-0.01)]; TO_MATCH_ENVRCPT_ALL(0.00)[]; NEURAL_SPAM_SHORT(0.75)[0.755,0]; DMARC_NA(0.00)[web.de]; NEURAL_SPAM_MEDIUM(0.20)[0.202,0]; RCPT_COUNT_ONE(0.00)[1]; DWL_DNSWL_LOW(-1.00)[web.de.dwl.dnswl.org : 127.0.5.1]; NEURAL_SPAM_LONG(0.49)[0.490,0]; FROM_NO_DN(0.00)[]; MIME_HTML_ONLY(0.20)[]; MID_RHS_NOT_FQDN(0.50)[]; RCVD_COUNT_TWO(0.00)[2] MIME-Version: 1.0 Content-Type: text/plain; charset="UTF-8" X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 22:23:41 -0000 From owner-freebsd-arm@freebsd.org Thu Jan 31 23:06:37 2019 Return-Path: Delivered-To: freebsd-arm@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 5A2DD14BB3B0 for ; Thu, 31 Jan 2019 23:06:37 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from mxrelay.ysv.freebsd.org (mxrelay.ysv.freebsd.org [IPv6:2001:1900:2254:206a::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.ysv.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id D068F800CA for ; Thu, 31 Jan 2019 23:06:36 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org (kenobi.freebsd.org [IPv6:2001:1900:2254:206a::16:76]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.ysv.freebsd.org (Postfix) with ESMTPS id 232A212825 for ; Thu, 31 Jan 2019 23:06:36 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org ([127.0.1.118]) by kenobi.freebsd.org (8.15.2/8.15.2) with ESMTP id x0VN6aes094446 for ; Thu, 31 Jan 2019 23:06:36 GMT (envelope-from bugzilla-noreply@freebsd.org) Received: (from www@localhost) by kenobi.freebsd.org (8.15.2/8.15.2/Submit) id x0VN6adA094445 for freebsd-arm@FreeBSD.org; Thu, 31 Jan 2019 23:06:36 GMT (envelope-from bugzilla-noreply@freebsd.org) X-Authentication-Warning: kenobi.freebsd.org: www set sender to bugzilla-noreply@freebsd.org using -f From: bugzilla-noreply@freebsd.org To: freebsd-arm@FreeBSD.org Subject: [Bug 235362] Cannot boot Jetson TK1 on FreeBSD 13.0-CURRENT Date: Thu, 31 Jan 2019 23:06:35 +0000 X-Bugzilla-Reason: AssignedTo X-Bugzilla-Type: new X-Bugzilla-Watch-Reason: None X-Bugzilla-Product: Base System X-Bugzilla-Component: arm X-Bugzilla-Version: CURRENT X-Bugzilla-Keywords: X-Bugzilla-Severity: Affects Only Me X-Bugzilla-Who: gndaryee@uwaterloo.ca X-Bugzilla-Status: New X-Bugzilla-Resolution: X-Bugzilla-Priority: --- X-Bugzilla-Assigned-To: freebsd-arm@FreeBSD.org X-Bugzilla-Flags: X-Bugzilla-Changed-Fields: bug_id short_desc product version rep_platform op_sys bug_status bug_severity priority component assigned_to reporter attachments.mimetype attachments.created Message-ID: Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: https://bugs.freebsd.org/bugzilla/ Auto-Submitted: auto-generated MIME-Version: 1.0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 23:06:37 -0000 https://bugs.freebsd.org/bugzilla/show_bug.cgi?id=3D235362 Bug ID: 235362 Summary: Cannot boot Jetson TK1 on FreeBSD 13.0-CURRENT Product: Base System Version: CURRENT Hardware: arm OS: Any Status: New Severity: Affects Only Me Priority: --- Component: arm Assignee: freebsd-arm@FreeBSD.org Reporter: gndaryee@uwaterloo.ca Attachment #201568 text/plain mime type: Created attachment 201568 --> https://bugs.freebsd.org/bugzilla/attachment.cgi?id=3D201568&action= =3Dedit Error log with printf statements showing lock state before initializing Kernel crashes during boot when booting a Jetson TK1 from NFS. Booting the kernel dies early on with "vm reserv" already initialized. Further investigation seems to show that not all of the mutexes used in the array were initialized to zero correctly. Using git bisect, it appears the commit that brought in the issue is base r340337 which brought in Linux devicetree specifications. After isolating the changes to the Jetson TK1, it appears that the memory region may be too big? Using a smaller length (256MB smaller) appears to resolve the issue. --=20 You are receiving this mail because: You are the assignee for the bug.= From owner-freebsd-arm@freebsd.org Thu Jan 31 23:21:52 2019 Return-Path: Delivered-To: freebsd-arm@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 D0A0C14BBA2C for ; Thu, 31 Jan 2019 23:21:52 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from mxrelay.ysv.freebsd.org (mxrelay.ysv.freebsd.org [IPv6:2001:1900:2254:206a::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.ysv.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 20177809D8 for ; Thu, 31 Jan 2019 23:21:52 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org (kenobi.freebsd.org [IPv6:2001:1900:2254:206a::16:76]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.ysv.freebsd.org (Postfix) with ESMTPS id 5C88C129D2 for ; Thu, 31 Jan 2019 23:21:51 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org ([127.0.1.118]) by kenobi.freebsd.org (8.15.2/8.15.2) with ESMTP id x0VNLpj2027962 for ; Thu, 31 Jan 2019 23:21:51 GMT (envelope-from bugzilla-noreply@freebsd.org) Received: (from www@localhost) by kenobi.freebsd.org (8.15.2/8.15.2/Submit) id x0VNLpk4027958 for freebsd-arm@FreeBSD.org; Thu, 31 Jan 2019 23:21:51 GMT (envelope-from bugzilla-noreply@freebsd.org) X-Authentication-Warning: kenobi.freebsd.org: www set sender to bugzilla-noreply@freebsd.org using -f From: bugzilla-noreply@freebsd.org To: freebsd-arm@FreeBSD.org Subject: [Bug 235363] Hard coded bcm2835 framebuffer bpp breaks Qt QImage Date: Thu, 31 Jan 2019 23:21:51 +0000 X-Bugzilla-Reason: AssignedTo X-Bugzilla-Type: new X-Bugzilla-Watch-Reason: None X-Bugzilla-Product: Base System X-Bugzilla-Component: arm X-Bugzilla-Version: 12.0-RELEASE X-Bugzilla-Keywords: X-Bugzilla-Severity: Affects Only Me X-Bugzilla-Who: ssw01@mathistry.net X-Bugzilla-Status: New X-Bugzilla-Resolution: X-Bugzilla-Priority: --- X-Bugzilla-Assigned-To: freebsd-arm@FreeBSD.org X-Bugzilla-Flags: X-Bugzilla-Changed-Fields: bug_id short_desc product version rep_platform op_sys bug_status bug_severity priority component assigned_to reporter Message-ID: Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: https://bugs.freebsd.org/bugzilla/ Auto-Submitted: auto-generated MIME-Version: 1.0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 31 Jan 2019 23:21:53 -0000 https://bugs.freebsd.org/bugzilla/show_bug.cgi?id=3D235363 Bug ID: 235363 Summary: Hard coded bcm2835 framebuffer bpp breaks Qt QImage Product: Base System Version: 12.0-RELEASE Hardware: arm64 OS: Any Status: New Severity: Affects Only Me Priority: --- Component: arm Assignee: freebsd-arm@FreeBSD.org Reporter: ssw01@mathistry.net --=20 You are receiving this mail because: You are the assignee for the bug.= From owner-freebsd-arm@freebsd.org Fri Feb 1 08:24:02 2019 Return-Path: Delivered-To: freebsd-arm@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 BFAC314BD9B7 for ; Fri, 1 Feb 2019 08:24:01 +0000 (UTC) (envelope-from doc.solo@web.de) Received: from mout.web.de (mout.web.de [212.227.15.14]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "mout.web.de", Issuer "TeleSec ServerPass DE-2" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 8C3EB77E9D for ; Fri, 1 Feb 2019 08:24:00 +0000 (UTC) (envelope-from doc.solo@web.de) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=web.de; s=dbaedf251592; t=1549009432; bh=uhe+khHz+FIj6NZNWR2zHuEcvbFHBRkSocR9HFhoIJE=; h=X-UI-Sender-Class:From:To:Cc:Subject:Date:In-Reply-To:References; b=MQN1FEl6E1so6Ldxr4Riyr/jJNTMdgxKdIFu9Td58T6aNuoLsKX18COto9ZZIVD2B ZYhlAwiOF4lKbWzr8W64OdL8gpeAXGXt4QgrWyKOHrQGA3yi9qBrW+uXEJ8J8N2lBq rhMtH6oOnViyylfua09Sb9X+FI2dG8ABgz38EB8Q= X-UI-Sender-Class: c548c8c5-30a9-4db5-a2e7-cb6cb037b8f9 Received: from [141.113.3.11] ([141.113.3.11]) by web-mail.web.de (3c-app-webde-bs50.server.lan [172.19.170.106]) (via HTTP); Fri, 1 Feb 2019 09:18:40 +0100 MIME-Version: 1.0 Message-ID: From: doc.solo@web.de To: "Marcin Wojtas" Cc: freebsd-arm Subject: Aw: Re: Help getting Marvell-A388 SBC booted Content-Type: text/plain; charset=UTF-8 Date: Fri, 1 Feb 2019 09:18:40 +0100 Importance: normal Sensitivity: Normal In-Reply-To: References: Content-Transfer-Encoding: quoted-printable X-UI-Message-Type: mail X-Priority: 3 X-Provags-ID: V03:K1:7xCcUUsZm/gHbs8hgnogc2OO2edBdHCm+lHxVojb9XNx5A8EnEwaz8GBgpxlCzUe+itFd 0Is+qCsF5IYzYq4QjRcGjBchNEm9giQDSF1Teu3EE0Hiddx5X7UwKTN2RPjVWX8905Ao/dKPLqJb a+VejG8nPWlbAsE5Va2eKUhBhjAvuKWM9HX83mLrNHpRxqL+1HJlQl0Kft/LYlVEsBEjgW2ADfK4 kAp9aZqjOyv67a78Etgo/pM0tuqJuWTNnReVudivHvmRSq6ld5TkzDhGfSoRtFumsHzdNtCgExiM t8= X-Spam-Flag: NO X-UI-Out-Filterresults: notjunk:1;V03:K0:DTJgEDs6VQk=:uxCDLDOpOXuItl8fdeyNAj mlMggLQNeRh+WM4hbShNHWIFToRNfSzQyGA+qnZiKtGXGw+h9rpA9kt4YY1oJd6jm3D8zMwiU oNkxEygUT1qA6KzILtXTcQ7XmoLE4/QSAKWFhkZLZUiqvAM9ml6SgOqqnccnNlhaKxqGtRYa0 /J4sC21i20H2fLbXVfd4r+r/8IHSmcmoMkyRahHjdhuUOlIh+1LYtJKOvjUPACwl3usfRxf68 7t4UOSbM8eXrktSRVW817RuFmWJexe2QN9xBNWHlzhwAvVMR1k6tLWh8IAZciYphV7Hagq3HS L5albceTFxTGNwNS+maNzETODpbl7IjZx3LYWursDHlYDN+YIS9y00Chu5O1iDLyg02+QPBrg cT4FmZfrz6w+ew9fqHrr/osPjcZB47meJJHrmNPmixcaXaQpSqI6nVBikvNeSUzT+XFpbiB4k TTdv0I/wS9bNcRGmO8Il20Duf+zECM6xvGvisqxQrYU4bfhFHnxj4w6qTY5RnIwyb3TnXXj9I jXo5w3aqaNdP+jB5XFEeq5QZi7MPKoQFr/W64lqmCJ3Z1/t5MXjBsqfnviFWMRyyHW4NI4BvH /x+bcYZMUPhMw= X-Rspamd-Queue-Id: 8C3EB77E9D X-Spamd-Bar: - Authentication-Results: mx1.freebsd.org; dkim=pass header.d=web.de header.s=dbaedf251592 header.b=MQN1FEl6; spf=pass (mx1.freebsd.org: domain of doc.solo@web.de designates 212.227.15.14 as permitted sender) smtp.mailfrom=doc.solo@web.de X-Spamd-Result: default: False [-1.10 / 15.00]; R_SPF_ALLOW(-0.20)[+ip4:212.227.15.0/25]; FREEMAIL_FROM(0.00)[web.de]; TO_DN_ALL(0.00)[]; DKIM_TRACE(0.00)[web.de:+]; MX_GOOD(-0.01)[cached: mx-ha02.web.de]; HAS_X_PRIO_THREE(0.00)[3]; RCPT_COUNT_TWO(0.00)[2]; FROM_EQ_ENVFROM(0.00)[]; RCVD_TLS_LAST(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_IN_DNSWL_LOW(-0.10)[14.15.227.212.list.dnswl.org : 127.0.5.1]; ASN(0.00)[asn:8560, ipnet:212.227.0.0/16, country:DE]; FREEMAIL_ENVFROM(0.00)[web.de]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-0.44)[-0.436,0]; R_DKIM_ALLOW(-0.20)[web.de:s=dbaedf251592]; IP_SCORE(0.26)[ipnet: 212.227.0.0/16(-0.76), asn: 8560(2.08), country: DE(-0.01)]; NEURAL_SPAM_SHORT(0.86)[0.862,0]; NEURAL_HAM_LONG(-0.68)[-0.677,0]; MIME_GOOD(-0.10)[text/plain]; DMARC_NA(0.00)[web.de]; DWL_DNSWL_LOW(-1.00)[web.de.dwl.dnswl.org : 127.0.5.1]; TO_MATCH_ENVRCPT_SOME(0.00)[]; FROM_NO_DN(0.00)[]; MID_RHS_NOT_FQDN(0.50)[]; RCVD_COUNT_TWO(0.00)[2] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 01 Feb 2019 08:24:02 -0000 Hi Marcin, =20 I used this device tree: https://github=2Ecom/Artox/crochet/blob/pr-clearf= og/board/Clearfog/files/armada-388-helios4=2Edts=2E I did a crochet build o= f FreeBSD-12 with config from above mentioned github repo=2E =20 I will build everything from scratch now, but documentation is really spar= se=2E So I still don't know what is really important to get FBSD booted=2E = My understanding is, that U-Boot needs the API enabled and that there are s= ome deviations from the linux device trees=2E Anything else? =20 BTW: Thanks to you and your colleagues for your work on the kernel to supp= ort this hardware=2E I wonder why this has remained largely unappreciated= =2E =20 Regards, =20 S=C3=B6ren From owner-freebsd-arm@freebsd.org Fri Feb 1 09:04:01 2019 Return-Path: Delivered-To: freebsd-arm@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 D757914C3472 for ; Fri, 1 Feb 2019 09:04:00 +0000 (UTC) (envelope-from mw@semihalf.com) Received: from mail-qt1-x82f.google.com (mail-qt1-x82f.google.com [IPv6:2607:f8b0:4864:20::82f]) (using TLSv1.2 with cipher ECDHE-RSA-AES128-GCM-SHA256 (128/128 bits)) (Client CN "smtp.gmail.com", Issuer "Google Internet Authority G3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 0C42F826AE for ; Fri, 1 Feb 2019 09:04:00 +0000 (UTC) (envelope-from mw@semihalf.com) Received: by mail-qt1-x82f.google.com with SMTP id v11so6653083qtc.2 for ; Fri, 01 Feb 2019 01:03:59 -0800 (PST) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=semihalf-com.20150623.gappssmtp.com; s=20150623; h=mime-version:references:in-reply-to:from:date:message-id:subject:to :cc:content-transfer-encoding; bh=MEArwP5e1O3Eeo5nLdUpfYuM5+S+0sEz7I4XdyftuHc=; b=LdGan4dLMdgXPS5kzPItW4mLB37iyypBTPNWreoe9dLZXpe9wgzeW3ZTh9GvbRruOa Tx7NB+3iSTbABCk0zqxQc0aUPdjLnonqbRyffX8Re5eTE5GNvbVYrW8tvGrymgTtji35 WhIdZQHLHEkRGq69EpUA/FDaiaFJr1u8FnDMkzXCaohSY6dKQHw5Z9+QX5sGco78YwYB lwB5ix2kZtFtg+/wz5UdZCq2I3invkgENnj6pvbWZ5dSDzkBZT8301dq2GEl2n+s5KmB UBqOAP9j1O2FP6G8eQll0SUcaGSLXwFmoqwAbWZSPTi98v/vNGwxXoam4fBvIugeAoB/ Cw3A== X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=1e100.net; s=20161025; h=x-gm-message-state:mime-version:references:in-reply-to:from:date :message-id:subject:to:cc:content-transfer-encoding; bh=MEArwP5e1O3Eeo5nLdUpfYuM5+S+0sEz7I4XdyftuHc=; b=DbQu3KY8Hsai1PV7IlOZ9yWI+A0dwtSpCHIsUHa7PNcguxv8FzjWoU7rOOaBVfLme8 WMZwWKrMfohR6QQHh9GOGx7neqnGJWdODW9EeJP1auH8gfkecJ2baKZeFWkWkVNFA48D SlECJ0DmX2UubBNPopFXRJmVomFnDVVNPT1bDvHU44pmHQj7FgqS95eUUxK/N/6rudoP c7w/8dHg8ORpEijTHNggFWpz7PZ11RfiwZNGkYkkc5uiD56AQepUsrdFpoqcKbrw5rmF 4HHNZBYMxeMxZ6iakxHVBRKHG0fILzX5A3Nao7rYhWFnM2GjZllN0nqgwZNgoLUmslAZ f+Wg== X-Gm-Message-State: AJcUukcg+J59duZpXSRgIY2CPG7E9BAbvztY7hOY6cSvKP2ywSKuIkpH B7eC0cAoJCsjmIVYfijmke0ViMO+XKSDuAJH0l/2UszmeEUPug== X-Google-Smtp-Source: ALg8bN7oqmrDAhcs7iamZDL+OqnQGR6lzpuXDDkzKC4nnZDwRKuxKM74q3tv2VrwQERsiqMLXH1nQSSXC9B42tvyJM8= X-Received: by 2002:a0c:9d41:: with SMTP id n1mr36175044qvf.212.1549011839321; Fri, 01 Feb 2019 01:03:59 -0800 (PST) MIME-Version: 1.0 References: In-Reply-To: From: Marcin Wojtas Date: Fri, 1 Feb 2019 10:03:48 +0100 Message-ID: Subject: Re: Re: Help getting Marvell-A388 SBC booted To: doc.solo@web.de Cc: freebsd-arm Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Rspamd-Queue-Id: 0C42F826AE X-Spamd-Bar: ----- Authentication-Results: mx1.freebsd.org; dkim=pass header.d=semihalf-com.20150623.gappssmtp.com header.s=20150623 header.b=LdGan4dL X-Spamd-Result: default: False [-5.60 / 15.00]; ARC_NA(0.00)[]; NEURAL_HAM_MEDIUM(-1.00)[-1.000,0]; R_DKIM_ALLOW(-0.20)[semihalf-com.20150623.gappssmtp.com:s=20150623]; FROM_HAS_DN(0.00)[]; TO_DN_SOME(0.00)[]; NEURAL_HAM_SHORT(-0.61)[-0.612,0]; NEURAL_HAM_LONG(-1.00)[-1.000,0]; MIME_GOOD(-0.10)[text/plain]; PREVIOUSLY_DELIVERED(0.00)[freebsd-arm@freebsd.org]; DMARC_NA(0.00)[semihalf.com]; TO_MATCH_ENVRCPT_SOME(0.00)[]; DKIM_TRACE(0.00)[semihalf-com.20150623.gappssmtp.com:+]; MX_GOOD(-0.01)[cached: ASPMX2.GOOGLEMAIL.com]; RCPT_COUNT_TWO(0.00)[2]; RCVD_IN_DNSWL_NONE(0.00)[f.2.8.0.0.0.0.0.0.0.0.0.0.0.0.0.0.2.0.0.4.6.8.4.0.b.8.f.7.0.6.2.list.dnswl.org : 127.0.5.0]; R_SPF_NA(0.00)[]; FREEMAIL_TO(0.00)[web.de]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+]; RCVD_TLS_LAST(0.00)[]; ASN(0.00)[asn:15169, ipnet:2607:f8b0::/32, country:US]; RCVD_COUNT_TWO(0.00)[2]; IP_SCORE(-2.68)[ip: (-8.87), ipnet: 2607:f8b0::/32(-2.49), asn: 15169(-1.95), country: US(-0.07)] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 01 Feb 2019 09:04:01 -0000 Hi S=C3=B6ren, pt., 1 lut 2019 o 09:18 napisa=C5=82(a): > > Hi Marcin, > > I used this device tree: https://github.com/Artox/crochet/blob/pr-clearfo= g/board/Clearfog/files/armada-388-helios4.dts. I did a crochet build of Fre= eBSD-12 with config from above mentioned github repo. > > I will build everything from scratch now, but documentation is really spa= rse. So I still don't know what is really important to get FBSD booted. My = understanding is, that U-Boot needs the API enabled and that there are some= deviations from the linux device trees. Anything else? We made an effort to remove all deviations from the Linux device trees, when adding support to GENERIC config. Therefore any customisation is no longer needed (it was added long time before 12 release). We also used unmodified u-boot from Marvell repos all the time. I need to check and help you (but not before the weekend :) ). > > BTW: Thanks to you and your colleagues for your work on the kernel to sup= port this hardware. I wonder why this has remained largely unappreciated. > Thanks. IMO the platform is in really good shape, both functionally and in terms of performance. Best regards, Marcin From owner-freebsd-arm@freebsd.org Fri Feb 1 15:14:33 2019 Return-Path: Delivered-To: freebsd-arm@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 E189114B6700 for ; Fri, 1 Feb 2019 15:14:32 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from mxrelay.ysv.freebsd.org (mxrelay.ysv.freebsd.org [IPv6:2001:1900:2254:206a::19:3]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) server-signature RSA-PSS (4096 bits) client-signature RSA-PSS (4096 bits) client-digest SHA256) (Client CN "mxrelay.ysv.freebsd.org", Issuer "Let's Encrypt Authority X3" (verified OK)) by mx1.freebsd.org (Postfix) with ESMTPS id 59CBD6C62C for ; Fri, 1 Feb 2019 15:14:32 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org (kenobi.freebsd.org [IPv6:2001:1900:2254:206a::16:76]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mxrelay.ysv.freebsd.org (Postfix) with ESMTPS id 083921B68C for ; Fri, 1 Feb 2019 15:14:31 +0000 (UTC) (envelope-from bugzilla-noreply@freebsd.org) Received: from kenobi.freebsd.org ([127.0.1.118]) by kenobi.freebsd.org (8.15.2/8.15.2) with ESMTP id x11FEUdp041543 for ; Fri, 1 Feb 2019 15:14:30 GMT (envelope-from bugzilla-noreply@freebsd.org) Received: (from www@localhost) by kenobi.freebsd.org (8.15.2/8.15.2/Submit) id x11FEUNM041535 for freebsd-arm@FreeBSD.org; Fri, 1 Feb 2019 15:14:30 GMT (envelope-from bugzilla-noreply@freebsd.org) X-Authentication-Warning: kenobi.freebsd.org: www set sender to bugzilla-noreply@freebsd.org using -f From: bugzilla-noreply@freebsd.org To: freebsd-arm@FreeBSD.org Subject: [Bug 235391] armv7: kernel.bin produced by buildkernel is corrupted. Date: Fri, 01 Feb 2019 15:14:30 +0000 X-Bugzilla-Reason: AssignedTo X-Bugzilla-Type: new X-Bugzilla-Watch-Reason: None X-Bugzilla-Product: Base System X-Bugzilla-Component: arm X-Bugzilla-Version: CURRENT X-Bugzilla-Keywords: X-Bugzilla-Severity: Affects Some People X-Bugzilla-Who: mmel@FreeBSD.org X-Bugzilla-Status: New X-Bugzilla-Resolution: X-Bugzilla-Priority: --- X-Bugzilla-Assigned-To: freebsd-arm@FreeBSD.org X-Bugzilla-Flags: X-Bugzilla-Changed-Fields: bug_id short_desc product version rep_platform op_sys bug_status bug_severity priority component assigned_to reporter Message-ID: Content-Type: text/plain; charset="UTF-8" Content-Transfer-Encoding: quoted-printable X-Bugzilla-URL: https://bugs.freebsd.org/bugzilla/ Auto-Submitted: auto-generated MIME-Version: 1.0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 01 Feb 2019 15:14:33 -0000 https://bugs.freebsd.org/bugzilla/show_bug.cgi?id=3D235391 Bug ID: 235391 Summary: armv7: kernel.bin produced by buildkernel is corrupted. Product: Base System Version: CURRENT Hardware: arm OS: Any Status: New Severity: Affects Some People Priority: --- Component: arm Assignee: freebsd-arm@FreeBSD.org Reporter: mmel@FreeBSD.org Actually, ld.lld changed many years lasting status quo - file layout of loadable sections in ELF file no longer correspond to in memory layout [1].= =20 Unfortunately, elftoolchain objcopy uses for generating kernel.bin images doesn't handle this well and produces invalid binary files. The generated binary follows ELF file layout, not a requested memory one. This changed ld.lld behavior also means that we cannot load kernel to memory and simply jump to start address to run it. Imo, many kernel developers use this technique in early stage of porting kernel to new HW. And I just noticed this, alignment of second load section looks very strang= e, I pretty sure that this is not a right output. [1] kernel generated by ld.lld: Program Headers: Type Offset VirtAddr PhysAddr FileSiz MemSiz Flg Align PHDR 0x000034 0xc0000034 0xc0000034 0x00120 0x00120 R 0x4 INTERP 0x730e6c 0xc0730e6c 0xc0730e6c 0x0000d 0x0000d R 0x1 [Requesting program interpreter: /red/herring] LOAD 0x000000 0xc0000000 0xc0000000 0x7f3804 0x7f3804 R E 0x1000 LOAD 0x7f3840 0xc07f4840 0xc07f4840 0xcf848 0x2f37c0 RW 0x4000 DYNAMIC 0x8c3040 0xc08c4040 0xc08c4040 0x00048 0x00048 RW 0x4 GNU_RELRO 0x8c3040 0xc08c4040 0xc08c4040 0x00048 0x00048 R 0x1 GNU_STACK 0x000000 0x00000000 0x00000000 0x00000 0x00000 RW 0 NOTE 0x7c102c 0xc07c102c 0xc07c102c 0x00024 0x00024 R 0x4 ARM_EXIDX 0x7d6774 0xc07d6774 0xc07d6774 0x1d090 0x1d090 R 0x4 exactly same (from identical objects) kernel generated by ld.bfd: Program Headers: Type Offset VirtAddr PhysAddr FileSiz MemSiz Flg Align ARM_EXIDX 0x7b7f10 0xc07b7f10 0xc07b7f10 0x1d3b0 0x1d3b0 R 0x4 PHDR 0x000034 0xc0000034 0xc0000034 0x000c0 0x000c0 R E 0x4 INTERP 0x72d188 0xc072d188 0xc072d188 0x0000d 0x0000d R 0x1 [Requesting program interpreter: /red/herring] LOAD 0x000000 0xc0000000 0xc0000000 0x8a5b0c 0xac8000 RWE 0x8000 DYNAMIC 0x8a5aa4 0xc08a5aa4 0xc08a5aa4 0x00068 0x00068 RW 0x4 GNU_STACK 0x000000 0x00000000 0x00000000 0x00000 0x00000 RWE 0x4 --=20 You are receiving this mail because: You are the assignee for the bug.= From owner-freebsd-arm@freebsd.org Fri Feb 1 22:24:13 2019 Return-Path: Delivered-To: freebsd-arm@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 56C0414C3058 for ; Fri, 1 Feb 2019 22:24:13 +0000 (UTC) (envelope-from fbsd@www.zefox.net) Received: from www.zefox.net (www.zefox.net [50.1.20.27]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client CN "www.zefox.org", Issuer "www.zefox.org" (not verified)) by mx1.freebsd.org (Postfix) with ESMTPS id 91FD585C9F for ; Fri, 1 Feb 2019 22:24:12 +0000 (UTC) (envelope-from fbsd@www.zefox.net) Received: from www.zefox.net (localhost [127.0.0.1]) by www.zefox.net (8.15.2/8.15.2) with ESMTPS id x11M83pd013263 (version=TLSv1.2 cipher=DHE-RSA-AES256-GCM-SHA384 bits=256 verify=NO); Fri, 1 Feb 2019 14:08:04 -0800 (PST) (envelope-from fbsd@www.zefox.net) Received: (from fbsd@localhost) by www.zefox.net (8.15.2/8.15.2/Submit) id x11M83H6013262; Fri, 1 Feb 2019 14:08:03 -0800 (PST) (envelope-from fbsd) Date: Fri, 1 Feb 2019 14:08:03 -0800 From: bob prohaska To: freebsd-arm@freebsd.org Subject: Regression testing buildworld on RPI3 Message-ID: <20190201220803.GA12071@www.zefox.net> MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline User-Agent: Mutt/1.5.24 (2015-08-30) X-Rspamd-Queue-Id: 91FD585C9F X-Spamd-Bar: ++++ Authentication-Results: mx1.freebsd.org X-Spamd-Result: default: False [4.74 / 15.00]; ARC_NA(0.00)[]; WWW_DOT_DOMAIN(0.50)[]; FROM_HAS_DN(0.00)[]; TO_DN_SOME(0.00)[]; NEURAL_SPAM_SHORT(0.74)[0.740,0]; IP_SCORE(0.24)[ip: (0.88), ipnet: 50.1.16.0/20(0.44), asn: 7065(-0.02), country: US(-0.07)]; MIME_GOOD(-0.10)[text/plain]; RCVD_TLS_LAST(0.00)[]; DMARC_NA(0.00)[zefox.net]; AUTH_NA(1.00)[]; NEURAL_SPAM_MEDIUM(0.95)[0.952,0]; RCVD_COUNT_THREE(0.00)[3]; TO_MATCH_ENVRCPT_SOME(0.00)[]; MX_GOOD(-0.01)[cached: www.zefox.net]; RCPT_COUNT_TWO(0.00)[2]; NEURAL_SPAM_LONG(0.91)[0.915,0]; R_SPF_NA(0.00)[]; FROM_EQ_ENVFROM(0.00)[]; R_DKIM_NA(0.00)[]; MIME_TRACE(0.00)[0:+]; ASN(0.00)[asn:7065, ipnet:50.1.16.0/20, country:US]; MID_RHS_MATCH_FROM(0.00)[]; MID_RHS_WWW(0.50)[] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 01 Feb 2019 22:24:13 -0000 After much trial by error, it's looking as if -j4 buildworld runs without error on r339376 and stops with signal 11 in cc somewhere near or after r342204. Can anybody suggest which individual revisions should be tested to locate a point of failure? Buildworld on a Pi3 takes about a day. Recovering from a failure, if it gets into userland, is much slower. I gather the problem is not apparent during a cross- compile on AMD64. The plan for now is to update, compile the kernel toolchain and a new kernel, then reboot and try to build world. IIUC this will exercise the new world without disturbing userland. Is this correct? If there's a failure, I can reboot the old kernel, back down the revision, and try again. Thanks for reading, and any thoughts. bob prohaska From owner-freebsd-arm@freebsd.org Fri Feb 1 23:52:29 2019 Return-Path: Delivered-To: freebsd-arm@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 C801414C5669 for ; Fri, 1 Feb 2019 23:52:29 +0000 (UTC) (envelope-from marklmi@yahoo.com) Received: from sonic315-14.consmr.mail.bf2.yahoo.com (sonic315-14.consmr.mail.bf2.yahoo.com [74.6.134.124]) (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 0DE5489C0E for ; Fri, 1 Feb 2019 23:52:28 +0000 (UTC) (envelope-from marklmi@yahoo.com) X-YMail-OSG: yFD_FSEVM1mgI1oaJOQTEOyejisLFfmlrbDmwmsnIdfhRrg9X.UXls0.MbBeEuI 4UquQ7rdNJSPG10Ry8sxYFiqYzqtJ61t4IVnzgHpIFyx1iGC9ZoASrqyZ.LUXwpTm873Y3bWtcz9 rXW7GLGg3Xg3SZKp4WOArfiKRDlXejsqSKB6I2nyUl3J4mrwu.D6ZnX3d.jVyL9y.oAm2yD0m2j5 aFjezplVndhMdueGV36gKMMnsnhdcku.KPOk1Y1G6MeT454XHDILLk.D7BQ_bcC6pN3IdZMtR3sm G_83JX3AMxxrm09kxJKD0dmb5OhWgAPO89FVI0C55.rW3AmR9vx8GL5cwLH.Or0zmyigAiVaT_wq 2egY5qVe9fPmj7fM7A.RozN9Wtu9qGomL68h9qvuPfp.6eOkBZ.VvQ1YM7cVQussOBunt.LIJRTm y_rQFUubWm0ouihBKrK8wSRii9h4ScDjZ_uv9ZUyoCrVT4wAJAxhZD0o7.LZny0xonb3Ak2XDUS1 he_tYLUUCe7YaOyErJ0pqOW2LaR77KRd1MEFgWBcBnLIHowkocpCG0Jxj9JIEoNqhq8Gyq4TtHIr ffcKwcIBoLhNRCZkagiPk5AqM9Mj_Vhq4Mq0GgAegDUU96V8wq7jfaexIGFadRNnlYIElHrz7_kh MtQoNf7At5CN_eSw3slP8pA5BP0ZxWTfDnQQFWyaY4hgpl8YrOvCfETjF_oBZ9f2vGtcal2Yn5Ac q7Es_9uTUcrch1sRZO_rFkk5DjjuPKKLoJ0JRPtlHu_dKnMBRRd0b1jAknzqx7ib0ecatGDrkBW1 jS9SVo4YsN2GH8WDHCcb_VLi2OAmIHezpk_PVzVVlzz19dRdq5SVcMJmYr3j_lruoqBDjtFggwe_ Df_ZAiOEBoRpDtFO.v3vRxn5XsSDmyOlFPUurLYTmyXlj7QdDLBozseO4wIhGzxVx0ohhljCRJka vdm2_IrtHjCiBNVijywbl1kEE4O2fDK1aofg92Qj2RjJGt3oY6Tap8tOB3mCFjZ4kkAOQXeVDGJQ ZOnSZlXqWI3spyDVomNo5M92OIQsuz0xjj1DO.BVs8SQocYHCUT011BG3lMpjTOwdLNv1_WNS Received: from sonic.gate.mail.ne1.yahoo.com by sonic315.consmr.mail.bf2.yahoo.com with HTTP; Fri, 1 Feb 2019 23:52:21 +0000 Received: from c-67-170-167-181.hsd1.or.comcast.net (EHLO [192.168.1.113]) ([67.170.167.181]) by smtp423.mail.bf1.yahoo.com (Oath Hermes SMTP Server) with ESMTPA ID f168bbe6f895ac44bf7ed489553a27a4; Fri, 01 Feb 2019 23:52:17 +0000 (UTC) Content-Type: text/plain; charset=us-ascii Mime-Version: 1.0 (Mac OS X Mail 12.2 \(3445.102.3\)) Subject: Re: RPI3 swap experiments ["was killed: out of swap space" with: "v_free_count: 5439, v_inactive_count: 1"] From: Mark Millard In-Reply-To: <20180809170900.GD68459@raichu> Date: Fri, 1 Feb 2019 15:52:15 -0800 Cc: bob prohaska , freebsd-arm@freebsd.org Content-Transfer-Encoding: 7bit Message-Id: <6348018B-D21D-409E-9AE0-44BE65A56BE7@yahoo.com> References: <6BFE7B77-A0E2-4FAF-9C68-81951D2F6627@yahoo.com> <20180802002841.GB99523@www.zefox.net> <20180802015135.GC99523@www.zefox.net> <20180806155837.GA6277@raichu> <20180808153800.GF26133@www.zefox.net> <20180808204841.GA19379@raichu> <20180809065648.GB30347@www.zefox.net> <20180809152152.GC68459@raichu> <915DFC7F-7AC9-484F-8619-C386FF077769@yahoo.com> <20180809170900.GD68459@raichu> To: Mark Johnston X-Mailer: Apple Mail (2.3445.102.3) X-Rspamd-Queue-Id: 0DE5489C0E X-Spamd-Bar: ++ X-Spamd-Result: default: False [2.10 / 15.00]; RCVD_VIA_SMTP_AUTH(0.00)[]; TO_DN_SOME(0.00)[]; R_SPF_ALLOW(-0.20)[+ptr:yahoo.com]; MV_CASE(0.50)[]; FREEMAIL_FROM(0.00)[yahoo.com]; RCVD_COUNT_THREE(0.00)[3]; MX_GOOD(-0.01)[cached: mta6.am0.yahoodns.net]; DKIM_TRACE(0.00)[yahoo.com:+]; DMARC_POLICY_ALLOW(-0.50)[yahoo.com,reject]; FROM_EQ_ENVFROM(0.00)[]; RCVD_TLS_LAST(0.00)[]; MIME_TRACE(0.00)[0:+]; FREEMAIL_ENVFROM(0.00)[yahoo.com]; ASN(0.00)[asn:26101, ipnet:74.6.128.0/21, country:US]; MID_RHS_MATCH_FROM(0.00)[]; DWL_DNSWL_NONE(0.00)[yahoo.com.dwl.dnswl.org : 127.0.5.0]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[yahoo.com:s=s2048]; FROM_HAS_DN(0.00)[]; RCPT_COUNT_THREE(0.00)[3]; NEURAL_SPAM_SHORT(0.96)[0.965,0]; MIME_GOOD(-0.10)[text/plain]; IP_SCORE(0.95)[ip: (2.27), ipnet: 74.6.128.0/21(1.41), asn: 26101(1.13), country: US(-0.07)]; NEURAL_SPAM_MEDIUM(0.62)[0.618,0]; TO_MATCH_ENVRCPT_SOME(0.00)[]; NEURAL_SPAM_LONG(0.08)[0.079,0]; RCVD_IN_DNSWL_NONE(0.00)[124.134.6.74.list.dnswl.org : 127.0.5.0] X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 01 Feb 2019 23:52:30 -0000 [Your old changes for reporting information no longer matches sys/vm/swap_pager.c as of head -r343030 and later.] On 2018-Aug-9, at 10:09, Mark Johnston wrote: > On Thu, Aug 09, 2018 at 09:21:38AM -0700, Mark Millard wrote: >> Would something like the patch that produced the messages >> like: >> >> waited 3s for async swap write >> waited 3s for swap buffer >> >> be appropriate as able to be enabled via a sysctl or in >> some other way? In other words: in the source code by standard, >> off by default, but able to be enabled without patching, >> possibly without rebuilding? > > Yes, I think so. We don't have a lot of visibility into the behaviour > of the pageout threads, and I have some ideas on how to improve that. > Swap I/O latency measurements are something I've wanted in the past. Your old changes for reporting information no longer matches sys/vm/swap_pager.c as of head -r343030 and later and nothing for this was merged into head or stable/12. Are you still planning to have an update for monitoring for such issues at some point? >> I ask because I've been thinking of having such on the >> FreeBSD's where I buildworld buildkernel and use poudriere-devel >> for port builds. It might warning me of marginal contexts and >> help explain any OOM kills that might occur. (Somethings >> things are difficult or time consuming to reproduce.) >> >> If monitored at the time, it might even help identify contexts >> that "machine-gun down requests" in environments were such can >> be a problem for swapping. === Mark Millard marklmi at yahoo.com ( dsl-only.net went away in early 2018-Mar) From owner-freebsd-arm@freebsd.org Sat Feb 2 23:59:31 2019 Return-Path: Delivered-To: freebsd-arm@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 67E6D14D4181 for ; Sat, 2 Feb 2019 23:59:31 +0000 (UTC) (envelope-from yamori813@yahoo.co.jp) Received: from nh605-vm10.bullet.mail.ssk.yahoo.co.jp (nh605-vm10.bullet.mail.ssk.yahoo.co.jp [182.22.90.83]) by mx1.freebsd.org (Postfix) with SMTP id 816956FF17 for ; Sat, 2 Feb 2019 23:59:18 +0000 (UTC) (envelope-from yamori813@yahoo.co.jp) Received: from [182.22.66.105] by nh605.bullet.mail.ssk.yahoo.co.jp with NNFMP; 02 Feb 2019 23:56:37 -0000 Received: from [182.22.91.131] by t603.bullet.mail.ssk.yahoo.co.jp with NNFMP; 02 Feb 2019 23:56:37 -0000 Received: from [127.0.0.1] by omp604.mail.ssk.yahoo.co.jp with NNFMP; 02 Feb 2019 23:56:37 -0000 X-Yahoo-Newman-Property: ymail-3 X-Yahoo-Newman-Id: 598996.30812.bm@omp604.mail.ssk.yahoo.co.jp X-YMail-OSG: Xrk6Uj4VM1lfcr7Vp0JYF6FlRtWk1CJIdGQ9dACCt_e3r9Xpqyo5XRsD0b_CH74 HSR.jhVnCKtyauyDeXgNqAyTsQr8w8q_kexFeUQwezKNuhreT7j8LAo7Qshf6aYrkkgUr8TCwRQU rkDhaE4gZJHysaMbH6gegGQneWfliLQ4g9TFIGlJLo.h9mr_9ZGfGzjH8By5ad3TF6tzRKAYu9N1 lNNcJp50EO.gVXK2jCEHB5Rs9W6Amr1VGIAG60QqrbPrhwwKDrAgjj5USh1WP5Ef1djvF9YA4iSw fe3th43Y9TkohDizAeCc.nOdGDdNDIkYDN7ZWWnW1jcxcBGAlOLZMWEHw4egYgMPJeVsMlSo.66H OAipwgxlQ37lc0d2g0LCXhiX5xj4C3UT2MIAlP3qU3_0KNLjadsJrKPGv..WZfEUMmRbLwRNZerS BXUugkGd2ZZZOXvJzqF2hKN2zp72ipU1SHxSMi06SM3qRGBQe.zX7oUsaW_ex8ys4FRicqzczoV5 PPHF1youoD.cZ1wq5bQ.nSIjT3b73n.3cK.h.qtBaHBUQ7oSQhfW37x0frKf2lUU36dEMGKTo1Zt sytTCOA3SP7mtpSyHOk1xexFoKaonoamC8E5A3NLp Received: from jws701102.mail.ssk.yahoo.co.jp by sendmailws618.mail.ssk.yahoo.co.jp; Sun, 03 Feb 2019 08:56:37 +0000; 1549151797.092 DKIM-Signature: v=1; a=rsa-sha256; q=dns/txt; c=relaxed/relaxed; t=1549151797; s=yj20110701; d=yahoo.co.jp; h=Date:From:Reply-To:To:Message-ID:Subject:MIME-Version:Content-Type:References; bh=TyPBwcJrYKN0m5MyM1Kuk62qdaJneRhmeH+emd7FgdE=; b=mSl1sZVq2yemXK8jDDgShd5TqFotbetJU6SfNEEp64CYfHHHRqWxeNbQzIMNci11 3lcPAeAuem6L+qg7FG1eCqDY+kEmm6ZDzi5SZsbPmYWvhHLFgZ3/c99vZqtfeqeVH0y /avxBZa63SwkTn9w58p0ajlyY5lItt+IOFNT122g= DomainKey-Signature: a=rsa-sha1; q=dns; c=nofws; s=yj20110701; d=yahoo.co.jp; h=Date:From:Reply-To:Message-ID:MIME-Version:Content-Type:References; b=hlME3HuU8SauSssA/zC7yGCvlWc5uO5n9FqS1NREVoqrXtofMOViHJtVv8o5GwyZ 5/uSNPH/QH8F2ux83+rgaytT46XgJSEvrtnt2B7FNx08mt2cxFLRydVA4ju8y52txel uFQyyxso9zfmJDNkKqvBlWwjTOf0je/wwfh/2Lgo=; X-yjpVirusScan: Scanned Date: Sun, 3 Feb 2019 08:56:36 +0900 (JST) From: Mori Hiroki Reply-To: Mori Hiroki To: "freebsd-arm@freebsd.org" Message-ID: <376232685.958030.1549151796353.JavaMail.yahoo@mail.yahoo.co.jp> Subject: build error MIME-Version: 1.0 References: <376232685.958030.1549151796353.JavaMail.yahoo.ref@mail.yahoo.co.jp> X-Rspamd-Queue-Id: 816956FF17 X-Spamd-Bar: +++ Authentication-Results: mx1.freebsd.org; dkim=pass header.d=yahoo.co.jp header.s=yj20110701 header.b=mSl1sZVq; spf=pass (mx1.freebsd.org: domain of yamori813@yahoo.co.jp designates 182.22.90.83 as permitted sender) smtp.mailfrom=yamori813@yahoo.co.jp X-Spamd-Result: default: False [3.26 / 15.00]; HAS_REPLYTO(0.00)[yamori813@yahoo.co.jp]; R_SPF_ALLOW(-0.20)[+ip4:182.22.90.0/23]; FREEMAIL_FROM(0.00)[yahoo.co.jp]; DKIM_TRACE(0.00)[yahoo.co.jp:+]; MX_GOOD(-0.01)[mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp,mx3.mail.yahoo.co.jp,mx5.mail.yahoo.co.jp,mx1.mail.yahoo.co.jp,mx2.mail.yahoo.co.jp]; RCVD_NO_TLS_LAST(0.10)[]; FROM_EQ_ENVFROM(0.00)[]; MIME_TRACE(0.00)[0:+,1:+]; FREEMAIL_ENVFROM(0.00)[yahoo.co.jp]; ASN(0.00)[asn:23816, ipnet:182.22.0.0/17, country:JP]; IP_SCORE(0.90)[ipnet: 182.22.0.0/17(2.55), asn: 23816(2.04), country: JP(-0.08)]; DWL_DNSWL_NONE(0.00)[yahoo.co.jp.dwl.dnswl.org : 127.0.5.0]; ARC_NA(0.00)[]; R_DKIM_ALLOW(-0.20)[yahoo.co.jp:s=yj20110701]; RCVD_COUNT_FIVE(0.00)[5]; FROM_HAS_DN(0.00)[]; REPLYTO_EQ_FROM(0.00)[]; TO_MATCH_ENVRCPT_ALL(0.00)[]; MIME_GOOD(-0.10)[multipart/alternative,text/plain]; FREEMAIL_REPLYTO(0.00)[yahoo.co.jp]; DMARC_NA(0.00)[yahoo.co.jp]; NEURAL_SPAM_MEDIUM(0.90)[0.901,0]; RCPT_COUNT_ONE(0.00)[1]; NEURAL_SPAM_SHORT(0.93)[0.928,0]; NEURAL_SPAM_LONG(0.94)[0.936,0]; RCVD_IN_DNSWL_NONE(0.00)[83.90.22.182.list.dnswl.org : 127.0.5.0]; TO_DN_EQ_ADDR_ALL(0.00)[] Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: quoted-printable X-Content-Filtered-By: Mailman/MimeDel 2.1.29 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.29 Precedence: list List-Id: "Porting FreeBSD to ARM processors." List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 02 Feb 2019 23:59:31 -0000 Hi I try to marvell kirkwood. I have build error on current. I use ZRouter build system. But almost FreeBSD cross build system. If you have advice please let me know. Thanks. Hiroki Mori -------------------------------------------------------------- >>> stage 3: cross tools -------------------------------------------------------------- cd /usr/home/hiroki/freebsd; INSTALL=3D"sh /usr/home/hiroki/freebsd/tools/i= nstall. sh"=C2=A0 TOOLS_PREFIX=3D/usr/home/hiroki/zobj/usr/home/hiroki/ZRouter/tmp/= usr/home/hir oki/freebsd/arm.arm/tmp=C2=A0 PATH=3D/usr/home/hiroki/zobj/usr/home/hiroki/= ZRouter/tmp/ usr/home/hiroki/freebsd/arm.arm/tmp/legacy/usr/sbin:/usr/home/hiroki/zobj/u= sr/ho me/hiroki/ZRouter/tmp/usr/home/hiroki/freebsd/arm.arm/tmp/legacy/usr/bin:/u= sr/ho me/hiroki/zobj/usr/home/hiroki/ZRouter/tmp/usr/home/hiroki/freebsd/arm.arm/= tmp/l egacy/bin:/sbin:/bin:/usr/sbin:/usr/bin=C2=A0 WORLDTMP=3D/usr/home/hiroki/z= obj/usr/home /hiroki/ZRouter/tmp/usr/home/hiroki/freebsd/arm.arm/tmp=C2=A0 MAKEFLAGS=3D"= -m /usr/home /hiroki/freebsd/tools/build/mk=C2=A0 -D NO_CLEAN -m /usr/home/hiroki/freebs= d/share/mk " make=C2=A0 -f Makefile.inc1=C2=A0 DESTDIR=3D=C2=A0 OBJTOP=3D'/usr/home/hi= roki/zobj/usr/home/hirok i/ZRouter/tmp/usr/home/hiroki/freebsd/arm.arm/tmp/obj-tools'=C2=A0 OBJROOT= =3D'${OBJTOP} /'=C2=A0 MAKEOBJDIRPREFIX=3D=C2=A0 BOOTSTRAPPING=3D1102000=C2=A0 BWPHASE=3D= cross-tools=C2=A0 SSP_CFLAGS=3D=C2=A0=20 MK_HTML=3Dno NO_LINT=3Dyes MK_MAN=3Dno=C2=A0 -DNO_PIC MK_PROFILE=3Dno -DNO_= SHARED=C2=A0 -DNO_CPU_C FLAGS MK_WARNS=3Dno MK_CTF=3Dno=C2=A0 MK_CLANG_EXTRAS=3Dno MK_CLANG_FULL=3D= no=C2=A0 MK_LLDB=3Dno MK_ RETPOLINE=3Dno MK_TESTS=3Dno=C2=A0 MK_INCLUDES=3Dyes MK_LLVM_TARGET_ALL=3Dn= o=C2=A0 TARGET=3Darm TARG ET_ARCH=3Darm=C2=A0 MK_GDB=3Dno MK_TESTS=3Dno cross-tools =3D=3D=3D> lib/clang (obj,all,install) =3D=3D=3D> lib/clang/libllvm (obj) =3D=3D=3D> lib/clang/libclang (obj) =3D=3D=3D> lib/clang/headers (obj) =3D=3D=3D> lib/clang/libllvm (all) =3D=3D=3D> lib/clang/libclang (all) =3D=3D=3D> lib/clang/headers (all) =3D=3D=3D> lib/clang/libllvm (install) =3D=3D=3D> lib/clang/libclang (install) =3D=3D=3D> lib/clang/headers (install) sh /usr/home/hiroki/freebsd/tools/install.sh=C2=A0 -C -o root -g wheel -m 4= 44=C2=A0 /usr/h ome/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/__clang_cuda_builti= n_var s.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/__clang_c= uda_c math.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/__clan= g_cud a_complex_builtins.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/= Heade rs/__clang_cuda_device_functions.h /usr/home/hiroki/freebsd/contrib/llvm/to= ols/c lang/lib/Headers/__clang_cuda_intrinsics.h /usr/home/hiroki/freebsd/contrib= /llvm /tools/clang/lib/Headers/__clang_cuda_libdevice_declares.h /usr/home/hiroki= /free bsd/contrib/llvm/tools/clang/lib/Headers/__clang_cuda_math_forward_declares= .h /u sr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/__clang_cuda_ru= ntime _wrapper.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/__= stdde f_max_align_t.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Heade= rs/__ wmmintrin_aes.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Heade= rs/__ wmmintrin_pclmul.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/He= aders /adxintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/= altiv ec.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/ammintri= n.h / usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/arm64intr.h /u= sr/ho me/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/arm_acle.h /usr/home= /hiro ki/freebsd/contrib/llvm/tools/clang/lib/Headers/armintr.h /usr/home/hiroki/= freeb sd/contrib/llvm/tools/clang/lib/Headers/avx2intrin.h /usr/home/hiroki/freeb= sd/co ntrib/llvm/tools/clang/lib/Headers/avx512bitalgintrin.h /usr/home/hiroki/fr= eebsd /contrib/llvm/tools/clang/lib/Headers/avx512bwintrin.h /usr/home/hiroki/fre= ebsd/ contrib/llvm/tools/clang/lib/Headers/avx512cdintrin.h /usr/home/hiroki/free= bsd/c ontrib/llvm/tools/clang/lib/Headers/avx512dqintrin.h /usr/home/hiroki/freeb= sd/co ntrib/llvm/tools/clang/lib/Headers/avx512erintrin.h /usr/home/hiroki/freebs= d/con trib/llvm/tools/clang/lib/Headers/avx512fintrin.h /usr/home/hiroki/freebsd/= contr ib/llvm/tools/clang/lib/Headers/avx512ifmaintrin.h /usr/home/hiroki/freebsd= /cont rib/llvm/tools/clang/lib/Headers/avx512ifmavlintrin.h /usr/home/hiroki/free= bsd/c ontrib/llvm/tools/clang/lib/Headers/avx512pfintrin.h /usr/home/hiroki/freeb= sd/co ntrib/llvm/tools/clang/lib/Headers/avx512vbmi2intrin.h /usr/home/hiroki/fre= ebsd/ contrib/llvm/tools/clang/lib/Headers/avx512vbmiintrin.h /usr/home/hiroki/fr= eebsd /contrib/llvm/tools/clang/lib/Headers/avx512vbmivlintrin.h /usr/home/hiroki= /free bsd/contrib/llvm/tools/clang/lib/Headers/avx512vlbitalgintrin.h /usr/home/h= iroki /freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vlbwintrin.h /usr/home/= hirok i/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vlcdintrin.h /usr/home= /hiro ki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vldqintrin.h /usr/hom= e/hir oki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vlintrin.h /usr/home= /hiro ki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vlvbmi2intrin.h /usr/= home/ hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vlvnniintrin.h /u= sr/ho me/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vnniintrin.h /= usr/h ome/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vpopcntdqintr= in.h=20 /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/avx512vpopcnt= dqvli ntrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/avxin= trin. h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/bmi2intrin.= h /us r/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/bmiintrin.h /usr= /home /hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/cetintrin.h /usr/home/= hirok i/freebsd/contrib/llvm/tools/clang/lib/Headers/cldemoteintrin.h /usr/home/h= iroki /freebsd/contrib/llvm/tools/clang/lib/Headers/clflushoptintrin.h /usr/home/= hirok i/freebsd/contrib/llvm/tools/clang/lib/Headers/clwbintrin.h /usr/home/hirok= i/fre ebsd/contrib/llvm/tools/clang/lib/Headers/clzerointrin.h /usr/home/hiroki/f= reebs d/contrib/llvm/tools/clang/lib/Headers/cpuid.h /usr/home/hiroki/freebsd/con= trib/ llvm/tools/clang/lib/Headers/emmintrin.h /usr/home/hiroki/freebsd/contrib/l= lvm/t ools/clang/lib/Headers/f16cintrin.h /usr/home/hiroki/freebsd/contrib/llvm/t= ools/ clang/lib/Headers/fma4intrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/= clang /lib/Headers/fmaintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/= lib/H eaders/fxsrintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/H= eader s/gfniintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Header= s/htm intrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/htmx= lintr in.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/ia32intr= in.h=20 /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/immintrin.h /= usr/h ome/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/invpcidintrin.h /us= r/hom e/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/lwpintrin.h /usr/home= /hiro ki/freebsd/contrib/llvm/tools/clang/lib/Headers/lzcntintrin.h /usr/home/hir= oki/f reebsd/contrib/llvm/tools/clang/lib/Headers/mm3dnow.h /usr/home/hiroki/free= bsd/c ontrib/llvm/tools/clang/lib/Headers/mm_malloc.h /usr/home/hiroki/freebsd/co= ntrib /llvm/tools/clang/lib/Headers/mmintrin.h /usr/home/hiroki/freebsd/contrib/l= lvm/t ools/clang/lib/Headers/module.modulemap /usr/home/hiroki/freebsd/contrib/ll= vm/to ols/clang/lib/Headers/movdirintrin.h /usr/home/hiroki/freebsd/contrib/llvm/= tools /clang/lib/Headers/msa.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/= lib/H eaders/mwaitxintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib= /Head ers/nmmintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Heade= rs/op encl-c.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/pcon= figin trin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/pkuint= rin.h =C2=A0/usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/pmmintr= in.h /usr/ home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/popcntintrin.h /us= r/hom e/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/prfchwintrin.h /usr/h= ome/h iroki/freebsd/contrib/llvm/tools/clang/lib/Headers/ptwriteintrin.h /usr/hom= e/hir oki/freebsd/contrib/llvm/tools/clang/lib/Headers/rdseedintrin.h /usr/home/h= iroki /freebsd/contrib/llvm/tools/clang/lib/Headers/rtmintrin.h /usr/home/hiroki/= freeb sd/contrib/llvm/tools/clang/lib/Headers/s390intrin.h /usr/home/hiroki/freeb= sd/co ntrib/llvm/tools/clang/lib/Headers/sgxintrin.h /usr/home/hiroki/freebsd/con= trib/ llvm/tools/clang/lib/Headers/shaintrin.h /usr/home/hiroki/freebsd/contrib/l= lvm/t ools/clang/lib/Headers/smmintrin.h /usr/home/hiroki/freebsd/contrib/llvm/to= ols/c lang/lib/Headers/tbmintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/cl= ang/l ib/Headers/tmmintrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/li= b/Hea ders/vadefs.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers= /vaes intrin.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/veci= ntrin .h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/vpclmulqdq= intri n.h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/waitpkgin= trin. h /usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/wbnoinvdint= rin.h =C2=A0/usr/home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/wmmintr= in.h /usr/ home/hiroki/freebsd/contrib/llvm/tools/clang/lib/Headers/x86intrin.h /usr/h= ome/h iroki/freebsd/contrib/llvm/tools/clang/lib/Headers/xmmintrin.h /usr/home/hi= roki/ freebsd/contrib/llvm/tools/clang/lib/Headers/xopintrin.h /usr/home/hiroki/f= reebs d/contrib/llvm/tools/clang/lib/Headers/xsavecintrin.h /usr/home/hiroki/free= bsd/c ontrib/llvm/tools/clang/lib/Headers/xsaveintrin.h /usr/home/hiroki/freebsd/= contr ib/llvm/tools/clang/lib/Headers/xsaveoptintrin.h /usr/home/hiroki/freebsd/c= ontri b/llvm/tools/clang/lib/Headers/xsavesintrin.h /usr/home/hiroki/freebsd/cont= rib/l lvm/tools/clang/lib/Headers/xtestintrin.h arm_fp16.h arm_neon.h /usr/home/h= iroki /zobj/usr/home/hiroki/ZRouter/tmp/usr/home/hiroki/freebsd/arm.arm/tmp/usr/l= ib/cl ang/7.0.1/include/ install: target directory `/usr/home/hiroki/zobj/usr/home/hiroki/ZRouter/tm= p/usr /home/hiroki/freebsd/arm.arm/tmp/usr/lib/clang/7.0.1/include/' does not exi= st