From owner-freebsd-arm@FreeBSD.ORG Sun Jun 16 22:10:01 2013 Return-Path: Delivered-To: freebsd-arm@smarthost.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id B8751276 for ; Sun, 16 Jun 2013 22:10:01 +0000 (UTC) (envelope-from gnats@FreeBSD.org) Received: from freefall.freebsd.org (freefall.freebsd.org [IPv6:2001:1900:2254:206c::16:87]) by mx1.freebsd.org (Postfix) with ESMTP id 8FC311BA7 for ; Sun, 16 Jun 2013 22:10:01 +0000 (UTC) Received: from freefall.freebsd.org (localhost [127.0.0.1]) by freefall.freebsd.org (8.14.7/8.14.7) with ESMTP id r5GMA10Y031415 for ; Sun, 16 Jun 2013 22:10:01 GMT (envelope-from gnats@freefall.freebsd.org) Received: (from gnats@localhost) by freefall.freebsd.org (8.14.7/8.14.7/Submit) id r5GMA05N031413; Sun, 16 Jun 2013 22:10:00 GMT (envelope-from gnats) Date: Sun, 16 Jun 2013 22:10:00 GMT Message-Id: <201306162210.r5GMA05N031413@freefall.freebsd.org> To: freebsd-arm@FreeBSD.org Cc: From: Sreekanth Rupavatharam Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list Reply-To: Sreekanth Rupavatharam List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 16 Jun 2013 22:10:01 -0000 The following reply was made to PR arm/179561; it has been noted by GNATS. From: Sreekanth Rupavatharam To: hiren panchasara Cc: freebsd-gnats-submit@freebsd.org Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi Date: Sun, 16 Jun 2013 15:00:15 -0700 This is a multi-part message in MIME format. --------------010706070709090609030701 Content-Type: text/plain; charset=UTF-8; format=flowed Content-Transfer-Encoding: 7bit On 6/14/13 5:25 PM, hiren panchasara wrote: > Does this look similar?:http://www.freebsd.org/cgi/query-pr.cgi?pr=178495 > > FWIW, Clang got updated to release 3.3 a couple days back on HEAD. Not > sure if this is fixed in that version. > > cheers, > Hiren No, looks like the issue remains on today's revision of HEAD. On top of that looks like the kernel for raspberry pi is broken. It now hangs at Kernel args: (null). I used an older version of kernel and I get the same error when compiling pcre port. -S --------------010706070709090609030701 Content-Type: text/html; charset=UTF-8 Content-Transfer-Encoding: 7bit
On 6/14/13 5:25 PM, hiren panchasara wrote:
Does this look similar?: http://www.freebsd.org/cgi/query-pr.cgi?pr=178495
 
 FWIW, Clang got updated to release 3.3 a couple days back on HEAD. Not
 sure if this is fixed in that version.
 
 cheers,
 Hiren
No, looks like the issue remains on today's revision of HEAD. On top of that looks like the kernel for raspberry pi is broken. It now hangs at Kernel args: (null). I used an older version of kernel and I get the same error when compiling pcre port.

-S
--------------010706070709090609030701-- From owner-freebsd-arm@FreeBSD.ORG Sun Jun 16 23:01:32 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 17C3E200 for ; Sun, 16 Jun 2013 23:01:32 +0000 (UTC) (envelope-from f0andrey@gmail.com) Received: from mail-we0-x229.google.com (mail-we0-x229.google.com [IPv6:2a00:1450:400c:c03::229]) by mx1.freebsd.org (Postfix) with ESMTP id A89351D79 for ; Sun, 16 Jun 2013 23:01:31 +0000 (UTC) Received: by mail-we0-f169.google.com with SMTP id n57so1871915wev.14 for ; Sun, 16 Jun 2013 16:01:30 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; bh=0CNmOAKjwBAmDG893IuqXoTaUG/qK8zN8FTDj/pnTrs=; b=Dq5ugGEZ+yONoATtSQp3SzzeBmaH9MulEKeUppX0JkySbkCZc+Kk0Vr8HzKqD1biYe MhwcIWkY3tOIR5yXaLJeRlIvXnyvl5acUXVLh/3eJViJ0fCKRMcu8a9UwMSX2lrX+WWt +TZanuqFaHZCWYfJfHIO1vy9Vobxq3AUPdsMFfJ8qJa1WCy+mXkULpgSriH1/d3HrA9r vnVQPcWl/jGu1ptvE3y5SXFvubLfByw3f9njBtVsgVf+qdY9mnF0Yz+PEBfKGsculsxk BpYBGAdzBXtlVbCYAJcKrQhCu2B6EReA9nnawlglP4gobnjgzQ6f3Zqh2YUuvvyhfspl 4SBQ== MIME-Version: 1.0 X-Received: by 10.194.1.226 with SMTP id 2mr6505471wjp.91.1371423690806; Sun, 16 Jun 2013 16:01:30 -0700 (PDT) Received: by 10.194.240.132 with HTTP; Sun, 16 Jun 2013 16:01:30 -0700 (PDT) In-Reply-To: <201306162210.r5GMA05N031413@freefall.freebsd.org> References: <201306162210.r5GMA05N031413@freefall.freebsd.org> Date: Mon, 17 Jun 2013 03:01:30 +0400 Message-ID: Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi From: Andrey Fesenko To: Sreekanth Rupavatharam Content-Type: text/plain; charset=UTF-8 Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 16 Jun 2013 23:01:32 -0000 On Mon, Jun 17, 2013 at 2:10 AM, Sreekanth Rupavatharam wrote: > The following reply was made to PR arm/179561; it has been noted by GNATS. > > From: Sreekanth Rupavatharam > To: hiren panchasara > Cc: freebsd-gnats-submit@freebsd.org > Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi > Date: Sun, 16 Jun 2013 15:00:15 -0700 > > This is a multi-part message in MIME format. > --------------010706070709090609030701 > Content-Type: text/plain; charset=UTF-8; format=flowed > Content-Transfer-Encoding: 7bit > > On 6/14/13 5:25 PM, hiren panchasara wrote: > > Does this look similar?:http://www.freebsd.org/cgi/query-pr.cgi?pr=178495 > > > > FWIW, Clang got updated to release 3.3 a couple days back on HEAD. Not > > sure if this is fixed in that version. > > > > cheers, > > Hiren > No, looks like the issue remains on today's revision of HEAD. On top of > that looks like the kernel for raspberry pi is broken. It now hangs at > Kernel args: (null). I used an older version of kernel and I get the > same error when compiling pcre port. > I have successfully compiled the port to the RPi and # uname -a FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #0 r251584M: Mon Jun 10 01:06:22 MSK 2013 andrey@my_book.local:/home/andrey/obj/arm.armv6/usr/src/sys/RPI-B-IPv6 arm If you need to download a complete package with dependencies http://armv6.bsdnir.info/packages/All/ this host IPv6 only if you need IPv4 use gate for example http://www.sixxs.net/tools/gateway/ From owner-freebsd-arm@FreeBSD.ORG Mon Jun 17 00:12:21 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id AEE868C9 for ; Mon, 17 Jun 2013 00:12:21 +0000 (UTC) (envelope-from tim@kientzle.com) Received: from monday.kientzle.com (99-115-135-74.uvs.sntcca.sbcglobal.net [99.115.135.74]) by mx1.freebsd.org (Postfix) with ESMTP id 912B91FED for ; Mon, 17 Jun 2013 00:12:21 +0000 (UTC) Received: (from root@localhost) by monday.kientzle.com (8.14.4/8.14.4) id r5H0CFPC066589; Mon, 17 Jun 2013 00:12:15 GMT (envelope-from tim@kientzle.com) Received: from [192.168.2.123] (CiscoE3000 [192.168.1.65]) by kientzle.com with SMTP id 66xi8c5wccqufe8e5uzte7832e; Mon, 17 Jun 2013 00:12:15 +0000 (UTC) (envelope-from tim@kientzle.com) Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi Mime-Version: 1.0 (Apple Message framework v1283) Content-Type: text/plain; charset=us-ascii From: Tim Kientzle In-Reply-To: <201306162210.r5GMA05N031413@freefall.freebsd.org> Date: Sun, 16 Jun 2013 17:12:13 -0700 Content-Transfer-Encoding: quoted-printable Message-Id: References: <201306162210.r5GMA05N031413@freefall.freebsd.org> To: Sreekanth Rupavatharam X-Mailer: Apple Mail (2.1283) Cc: freebsd-arm@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 17 Jun 2013 00:12:21 -0000 On Jun 16, 2013, at 3:10 PM, Sreekanth Rupavatharam wrote: >=20 > On 6/14/13 5:25 PM, hiren panchasara wrote: >> Does this look = similar?:http://www.freebsd.org/cgi/query-pr.cgi?pr=3D178495 >>=20 >> FWIW, Clang got updated to release 3.3 a couple days back on HEAD. = Not >> sure if this is fixed in that version. >>=20 >> cheers, >> Hiren > No, looks like the issue remains on today's revision of HEAD. On top = of=20 > that looks like the kernel for raspberry pi is broken. It now hangs at=20= > Kernel args: (null). The "Kernel args:" line is the last thing printed by ubldr before transferring control to the kernel. If this is the last thing you see, then any of the following could be at issue: * ubldr could be broken, either not loading the kernel or not = transferring control properly. * kernel could be crashing in the early setup * kernel could be crashing in initarm (before the console is = initialized) If you can boot an older kernel with newer ubldr, then that would rule out ubldr breakage. Tim From owner-freebsd-arm@FreeBSD.ORG Mon Jun 17 01:22:34 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 8E32E56B for ; Mon, 17 Jun 2013 01:22:34 +0000 (UTC) (envelope-from rskanth@yahoo.com) Received: from nm33.bullet.mail.gq1.yahoo.com (nm33.bullet.mail.gq1.yahoo.com [98.136.217.16]) by mx1.freebsd.org (Postfix) with ESMTP id 49145120C for ; Mon, 17 Jun 2013 01:22:33 +0000 (UTC) Received: from [98.137.12.58] by nm33.bullet.mail.gq1.yahoo.com with NNFMP; 17 Jun 2013 01:22:33 -0000 Received: from [208.71.42.211] by tm3.bullet.mail.gq1.yahoo.com with NNFMP; 17 Jun 2013 01:22:33 -0000 Received: from [127.0.0.1] by smtp222.mail.gq1.yahoo.com with NNFMP; 17 Jun 2013 01:22:33 -0000 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=yahoo.com; s=s1024; t=1371432153; bh=bqHjPO8WYft+FdGBv30UPG2XP1AWNF0YkUphxvziWto=; h=X-Yahoo-Newman-Id:X-Yahoo-Newman-Property:X-YMail-OSG:X-Yahoo-SMTP:X-Rocket-Received:Message-ID:Date:From:User-Agent:MIME-Version:To:CC:Subject:References:In-Reply-To:Content-Type:Content-Transfer-Encoding; b=IR/aDWiyTTtUKZ15E4sJ+kffJf0COdxe4+ibLupaNR2rh1V0VGsN3VSGrPiMHysBoTzQCimykhRshWnn6/BOJWktrcQ3baMAlL8aJFJLt90OWLkNqVJNdWMlwkuS8pPJYmTS08ot4NnZSJ7Pjh9q2ruGX04+E3dXLaPOzRYKHnk= X-Yahoo-Newman-Id: 23721.25547.bm@smtp222.mail.gq1.yahoo.com X-Yahoo-Newman-Property: ymail-3 X-YMail-OSG: wgReCjUVM1mcmUwWuqovXT53JUnV4vlViSmII_S4UdLVo5W CjMPaJlIZRqpnhZFKrjqo9K97BFlpRo8VUUHx7VLJ5RAN_cjF.LL65fxfuy5 dUhN.oHPhcs9DlBJSGkwqNCVzRjEAIPXDAj7NDIIemWhjYDwLK5_KL3sKqo4 MaLjduN1p6QdLlLM8qMp9chpljnikGbcFFcDlq9fHXyMguNdMj2ojPM4elMJ HqJ2h8SiQUC1Nhoh5U33aKxJT1HiX39JKs1Scfgd2BvYG_4txl8xCdB_2cKG PUApbl747CEiUIS.vDhv5QnwMYngASIzIkm9Boq8dzV.lv_lxgSgTusKRy0K wB39pmDo4mIAa1NHdSXA44DoeixqHzICcXAmOD3yhHyyYRcLfs86Bl7eqPmD KeJAzexXKBDf.tTl39O9lwjPiF2gAFmJcpJtzGT46kpcdGTdme63Lm6aVeOp S3BBLVwo53dXr2JlFnzKont0KO9rIzVm15DPj2F7_a5cA3ZzKOCND5zoK4wu ifbg81uk- X-Yahoo-SMTP: 0vhBds2swBAUIWerZ77I22nIbgU- X-Rocket-Received: from sreekanth.voilavip.com (rskanth@24.130.110.113 with ) by smtp222.mail.gq1.yahoo.com with SMTP; 17 Jun 2013 01:22:32 +0000 UTC Message-ID: <51BE64D7.5010403@yahoo.com> Date: Sun, 16 Jun 2013 18:22:31 -0700 From: Sreekanth Rupavatharam User-Agent: Mozilla/5.0 (Macintosh; Intel Mac OS X 10.8; rv:17.0) Gecko/20130509 Thunderbird/17.0.6 MIME-Version: 1.0 To: Tim Kientzle Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi References: <201306162210.r5GMA05N031413@freefall.freebsd.org> In-Reply-To: Content-Type: text/plain; charset=ISO-8859-1; format=flowed Content-Transfer-Encoding: 7bit Cc: freebsd-arm@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 17 Jun 2013 01:22:34 -0000 On 6/16/13 5:12 PM, Tim Kientzle wrote: > If you can boot an older kernel with newer ubldr, then that > would rule out ubldr breakage. Yes, I confirmed that an older kernel with new image boots past the error. -S From owner-freebsd-arm@FreeBSD.ORG Mon Jun 17 11:06:41 2013 Return-Path: Delivered-To: freebsd-arm@FreeBSD.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id E6D4B17F for ; Mon, 17 Jun 2013 11:06:41 +0000 (UTC) (envelope-from owner-bugmaster@FreeBSD.org) Received: from freefall.freebsd.org (freefall.freebsd.org [IPv6:2001:1900:2254:206c::16:87]) by mx1.freebsd.org (Postfix) with ESMTP id C104B1BFE for ; Mon, 17 Jun 2013 11:06:41 +0000 (UTC) Received: from freefall.freebsd.org (localhost [127.0.0.1]) by freefall.freebsd.org (8.14.7/8.14.7) with ESMTP id r5HB6fIm012650 for ; Mon, 17 Jun 2013 11:06:41 GMT (envelope-from owner-bugmaster@FreeBSD.org) Received: (from gnats@localhost) by freefall.freebsd.org (8.14.7/8.14.7/Submit) id r5HB6fBO012648 for freebsd-arm@FreeBSD.org; Mon, 17 Jun 2013 11:06:41 GMT (envelope-from owner-bugmaster@FreeBSD.org) Date: Mon, 17 Jun 2013 11:06:41 GMT Message-Id: <201306171106.r5HB6fBO012648@freefall.freebsd.org> X-Authentication-Warning: freefall.freebsd.org: gnats set sender to owner-bugmaster@FreeBSD.org using -f From: FreeBSD bugmaster To: freebsd-arm@FreeBSD.org Subject: Current problem reports assigned to freebsd-arm@FreeBSD.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 17 Jun 2013 11:06:42 -0000 Note: to view an individual PR, use: http://www.freebsd.org/cgi/query-pr.cgi?pr=(number). The following is a listing of current problems submitted by FreeBSD users. These represent problem reports covering all versions including experimental development code and obsolete releases. S Tracker Resp. Description -------------------------------------------------------------------------------- o arm/179561 arm Compilation issue for lighttpd on raspberry pi o arm/179532 arm wireless networking on ARM o arm/178495 arm buildworld fail on arm/raspberry pi o arm/177687 arm gdb gets installed but does not know the EABI version o arm/177686 arm assertion failed in ld-elf.so.1 when invoking telnet w o arm/177685 arm [kernel] [patch] Correct return type and usage of at91 o arm/177538 arm tunefs(8) and mount(8) can not access a newfs(8)'d fil o arm/176424 arm Compiler warning, TARGET_ARCH=armv6, make MALLOC_PRODU o arm/175803 arm building xdev for arm failing o arm/175605 arm please fix build binutils-2.23.1 in raspberry pi o arm/174461 arm [patch] Fix off-by-one in arm9/arm10 cache maintenance o arm/173617 arm Dreamplug exhibits eSATA file corruption using network o kern/171096 arm [arm][xscale][ixp]Allow 16bit access on PCI bus o arm/166256 arm build fail in pmap.c o arm/162159 arm [panic] USB errors leading to panic on DockStar 9.0-RC o arm/161110 arm /usr/src/sys/arm/include/signal.h is bad o arm/161044 arm devel/icu does not build on arm o arm/158950 arm arm/sheevaplug fails fsx when mmap operations are enab o arm/155894 arm [patch] Enable at91 booting from SDHC (high capacity) p arm/155214 arm [patch] MMC/SD IO slow on Atmel ARM with modern large o arm/154227 arm [geli] using GELI leads to panic on ARM o arm/153380 arm Panic / translation fault with wlan on ARM o arm/150581 arm [irq] Unknown error generates IRQ address decoding err o arm/134368 arm [new driver] [patch] nslu2_led driver for the LEDs on p arm/134338 arm [patch] Lock GPIO accesses on ixp425 25 problems total. From owner-freebsd-arm@FreeBSD.ORG Mon Jun 17 20:52:10 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id D50CBEA8 for ; Mon, 17 Jun 2013 20:52:10 +0000 (UTC) (envelope-from rskanth@yahoo.com) Received: from nm9-vm6.bullet.mail.ne1.yahoo.com (nm9-vm6.bullet.mail.ne1.yahoo.com [98.138.91.102]) by mx1.freebsd.org (Postfix) with ESMTP id 716831F01 for ; Mon, 17 Jun 2013 20:52:10 +0000 (UTC) Received: from [98.138.226.177] by nm9.bullet.mail.ne1.yahoo.com with NNFMP; 17 Jun 2013 20:52:04 -0000 Received: from [98.138.226.129] by tm12.bullet.mail.ne1.yahoo.com with NNFMP; 17 Jun 2013 20:52:04 -0000 Received: from [127.0.0.1] by smtp216.mail.ne1.yahoo.com with NNFMP; 17 Jun 2013 20:52:04 -0000 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=yahoo.com; s=s1024; t=1371502324; bh=ULhc21ILjVR7iq/D+SNHC9E5iMcuRWVaT0lPP5BnnVM=; h=X-Yahoo-Newman-Id:X-Yahoo-Newman-Property:X-YMail-OSG:X-Yahoo-SMTP:X-Rocket-Received:Message-ID:Date:From:User-Agent:MIME-Version:To:CC:Subject:References:In-Reply-To:Content-Type:Content-Transfer-Encoding; b=E9ETxgeLBXvM4K2Pz/jGe50QiHaJs3YbHkuHh3WF87M0JSRzeC09Th6tBVKaFrMUPvxrwu6VDN3VYu6T5J0s1RngQlwNNbCrDSGn51O2VlykAPeAuJciammqAxuP4VXa+WCM/9nWG6Miyn8O0ScRz/3s0SpRAQjLtRvjYUjiXwM= X-Yahoo-Newman-Id: 312659.80901.bm@smtp216.mail.ne1.yahoo.com X-Yahoo-Newman-Property: ymail-3 X-YMail-OSG: 1ws_xpYVM1kN0eA_mGY7x.Xl6DGnsuOi6Apbvn2rGPgcM3q MrqlN.hRPYJ_nc1HdPhN7.EI6xyrLCrJIIYq9q5V_0nb4sHaqvoua5eTzy4o 4S3kjpSiF_juV7PUEVzR8d2263t0AuXaFC26xpldZlqr_.pIEX2nbsTbwNBh 2Q50vDRZwk7vwyJujwradRgIoybNFWAuD0UZ3sWeioUHXbHCeiACSb33aYwP tRO_wI3kpyVMASAHhN1hDzKXWaYH57XNc8EP4Dhs9uk9nOGGuEOPAs5ZBexm NEkrG3NFwm3U9yHRyVQqHRuwjPFoOYORZ0p9Jj6JdlesuO2OP1_9iiJUR2VA iwhol.7bojY6V2FhfFhM_zP3ETXdorRs4lgkrxSUOT8BwYr3VJJkCrlfyr99 SNK3mcOtQWCM4FdZ4LyVCG.Uu.V9nIGnorkgFA42A_XGOX8qAPtrgooL4Gq2 2ZWrNU6FJMoLpqPfGtBM3z3Tl8tdoJheDqUs6EDAVrX44pR4nyQ-- X-Yahoo-SMTP: 0vhBds2swBAUIWerZ77I22nIbgU- X-Rocket-Received: from sreekanth.voilavip.com (rskanth@24.130.110.113 with ) by smtp216.mail.ne1.yahoo.com with SMTP; 17 Jun 2013 13:52:04 -0700 PDT Message-ID: <51BF76F3.8020806@yahoo.com> Date: Mon, 17 Jun 2013 13:52:03 -0700 From: Sreekanth Rupavatharam User-Agent: Mozilla/5.0 (Macintosh; Intel Mac OS X 10.8; rv:17.0) Gecko/20130509 Thunderbird/17.0.6 MIME-Version: 1.0 To: Andrey Fesenko Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi References: <201306162210.r5GMA05N031413@freefall.freebsd.org> In-Reply-To: Content-Type: text/plain; charset=UTF-8; format=flowed Content-Transfer-Encoding: 7bit Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 17 Jun 2013 20:52:10 -0000 On 6/16/13 4:01 PM, Andrey Fesenko wrote: > I have successfully compiled the port to the RPi and > # uname -a > FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #0 r251584M: > Mon Jun 10 01:06:22 MSK 2013 > andrey@my_book.local:/home/andrey/obj/arm.armv6/usr/src/sys/RPI-B-IPv6 > arm I checked out the exact rev and built the image with that(with crochet-freebsd) and I still get the same issue with the C++ crashing 1. /usr/include/c++/4.2/bits/basic_string.tcc:978:43: current parser token ';' 2. /usr/include/c++/4.2/bits/basic_string.tcc:48:1 : parsing namespace 'std' c++: error: unable to execute command: Abort trap (core dumped) c++: error: clang frontend command failed due to signal (use -v to see invocation) FreeBSD clang version 3.3 (trunk 178860) 20130405 Target: armv6-unknown-freebsd10.0 Wonder what am I missing here My uname -a is #uname -a FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #0 r251584: Mon Jun 17 12:22:39 PDT 2013 root@voila1.voilavip.com:/b/raspberry/crochet-freebsd/work/obj/arm.armv6/b/raspberry/head/sys/RPI-B-WIFI arm From owner-freebsd-arm@FreeBSD.ORG Mon Jun 17 22:04:22 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 1E4A3C93 for ; Mon, 17 Jun 2013 22:04:22 +0000 (UTC) (envelope-from f0andrey@gmail.com) Received: from mail-wg0-x22c.google.com (mail-wg0-x22c.google.com [IPv6:2a00:1450:400c:c00::22c]) by mx1.freebsd.org (Postfix) with ESMTP id AEBE2128A for ; Mon, 17 Jun 2013 22:04:21 +0000 (UTC) Received: by mail-wg0-f44.google.com with SMTP id m15so2822532wgh.11 for ; Mon, 17 Jun 2013 15:04:20 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; bh=kWixIW5Vr36nfBYQfSo5OflTj7S0VYaIWbngWpdm1P8=; b=KDYSZbMOj3HazHpdO8OaMqW7LMNq6CXl8u6bpro53YNPjUu5tyIZKdEZmQW2V1AVXJ uHGsD0MU9T+Cwo0ZhZiaCoorgJRPTxkuqzjr62879Z+0ehZVurHRtYqjQloUSRL3zHkK 7lJMXdmhKX2JYuk36F6JXBUmtBItNZuLrdw3tP9GHatCCCXQew/i00uFXRDjJyLhwZAU jnZSxuxEOHGr/04xJOTdYlpjSkLPQAQm/J2QdEzv+SKsRNVQwsxq97K3fhkfNVx0atg9 t4UuO8kNSmP+yWycaiwi+0jQV2lRsnf6bM31ZmSYyEMLX17a2UmBznIMRKf/x/DWxilu loMw== MIME-Version: 1.0 X-Received: by 10.180.80.6 with SMTP id n6mr6062946wix.59.1371506660820; Mon, 17 Jun 2013 15:04:20 -0700 (PDT) Received: by 10.194.240.132 with HTTP; Mon, 17 Jun 2013 15:04:20 -0700 (PDT) In-Reply-To: <51BF76F3.8020806@yahoo.com> References: <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> Date: Tue, 18 Jun 2013 02:04:20 +0400 Message-ID: Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi From: Andrey Fesenko To: Sreekanth Rupavatharam Content-Type: text/plain; charset=UTF-8 Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 17 Jun 2013 22:04:22 -0000 On Tue, Jun 18, 2013 at 12:52 AM, Sreekanth Rupavatharam wrote: > On 6/16/13 4:01 PM, Andrey Fesenko wrote: >> >> I have successfully compiled the port to the RPi and >> # uname -a >> FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #0 r251584M: >> Mon Jun 10 01:06:22 MSK 2013 >> andrey@my_book.local:/home/andrey/obj/arm.armv6/usr/src/sys/RPI-B-IPv6 >> arm > > > I checked out the exact rev and built the image with that(with > crochet-freebsd) and I still get the same issue with the C++ crashing > > > > 1. /usr/include/c++/4.2/bits/basic_string.tcc:978:43: current parser > token ';' > 2. /usr/include/c++/4.2/bits/basic_string.tcc:48:1 > : parsing namespace > 'std' > c++: error: unable to execute command: Abort trap (core dumped) > c++: error: clang frontend command failed due to signal (use -v to see > invocation) > FreeBSD clang version 3.3 (trunk 178860) 20130405 > Target: armv6-unknown-freebsd10.0 > > Wonder what am I missing here > > My uname -a is > > #uname -a > FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #0 r251584: Mon Jun > 17 12:22:39 PDT 2013 > root@voila1.voilavip.com:/b/raspberry/crochet-freebsd/work/obj/arm.armv6/b/raspberry/head/sys/RPI-B-WIFI > arm i'm rebuild devel/pcre http://armv6.bsdnir.info.ipv4.sixxs.org/files/pcre_build.log are you build image on the system with blank /etc/make.conf? may be you build clang version # gcc -v Using built-in specs. Target: armv6-undermydesk-freebsd Configured with: FreeBSD/armv6 system compiler Thread model: posix gcc version 4.2.1 20070831 patched [FreeBSD] # g++ -v Using built-in specs. Target: armv6-undermydesk-freebsd Configured with: FreeBSD/armv6 system compiler Thread model: posix gcc version 4.2.1 20070831 patched [FreeBSD] or you RPi have /etc/make.conf with clang From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 02:21:25 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id B38E0E87 for ; Tue, 18 Jun 2013 02:21:25 +0000 (UTC) (envelope-from mcgovern@beta.com) Received: from spoon.beta.com (spoon.beta.com [199.165.180.2]) by mx1.freebsd.org (Postfix) with ESMTP id 653FB1FB4 for ; Tue, 18 Jun 2013 02:21:25 +0000 (UTC) Received: from [199.165.180.44] ([199.165.180.44]) by spoon.beta.com (8.14.5/8.14.5) with ESMTP id r5I2BEa2001045 for ; Mon, 17 Jun 2013 22:11:15 -0400 (EDT) (envelope-from mcgovern@beta.com) Subject: Two questions on -current... From: "Brian J. McGovern" To: freebsd-arm@freebsd.org In-Reply-To: References: Content-Type: text/plain; charset="us-ascii" Organization: B.E.T.A. Date: Mon, 17 Jun 2013 22:11:14 -0400 Message-ID: <1371521474.1391.9.camel@fbsd-laptop> Mime-Version: 1.0 X-Mailer: Evolution 2.32.1 FreeBSD GNOME Team Port Content-Transfer-Encoding: 7bit X-Spam-Status: No, score=1.3 required=5.0 tests=RDNS_NONE autolearn=no version=3.3.2 X-Spam-Level: * X-Spam-Checker-Version: SpamAssassin 3.3.2 (2011-06-06) on spoon.beta.com X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list Reply-To: mcgovern@beta.com List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 02:21:25 -0000 I'm currently using a fairly recent (within the week) -current on a Beaglebone Black and trying to use it on an OpenRD ultimate... I have two questions that I can't seem to find recent answers online. 1.) On the Beaglebone black, is there an interface for setting up the MUX on the GPIO pins? I've seen gpioctl, which doesn't seem to have the capability, and there seems to be settings in the DTS file, although it appears incomplete (e.g. not all pins are configured), but is there a way to dynamically set up the MUX during run time? 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: unknown target CPU 'armv5te', despite a find ... grep... on the code showing this option in both gcc and clang compilers and tools. Is this processor deprecated in current? Is there are a replacement? Did I miss a change in how to build the kernel (Currently using "make TARGET=arm TARGET_ARCH=arm KERNCONF=DB-88F6XXX buildkernel" in /usr/src)? -B From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 02:23:10 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 74C0BEFF; Tue, 18 Jun 2013 02:23:10 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id 398E21FC9; Tue, 18 Jun 2013 02:23:09 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5I2N9o7040416; Mon, 17 Jun 2013 22:23:09 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5I2N9S9040413; Tue, 18 Jun 2013 02:23:09 GMT (envelope-from tinderbox@freebsd.org) Date: Tue, 18 Jun 2013 02:23:09 GMT Message-Id: <201306180223.r5I2N9S9040413@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 02:23:10 -0000 TB --- 2013-06-17 22:50:17 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-17 22:50:17 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-17 22:50:17 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-17 22:50:17 - cleaning the object tree TB --- 2013-06-17 22:50:17 - /usr/local/bin/svn stat /src TB --- 2013-06-17 22:50:22 - At svn revision 251871 TB --- 2013-06-17 22:50:23 - building world TB --- 2013-06-17 22:50:23 - CROSS_BUILD_TESTING=YES TB --- 2013-06-17 22:50:23 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-17 22:50:23 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-17 22:50:23 - SRCCONF=/dev/null TB --- 2013-06-17 22:50:23 - TARGET=arm TB --- 2013-06-17 22:50:23 - TARGET_ARCH=arm TB --- 2013-06-17 22:50:23 - TZ=UTC TB --- 2013-06-17 22:50:23 - __MAKE_CONF=/dev/null TB --- 2013-06-17 22:50:23 - cd /src TB --- 2013-06-17 22:50:23 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Mon Jun 17 22:50:29 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools >>> stage 4.1: building includes >>> stage 4.2: building libraries >>> stage 4.3: make dependencies >>> stage 4.4: building everything >>> World build completed on Tue Jun 18 01:50:36 UTC 2013 TB --- 2013-06-18 01:50:36 - generating LINT kernel config TB --- 2013-06-18 01:50:36 - cd /src/sys/arm/conf TB --- 2013-06-18 01:50:36 - /usr/bin/make -B LINT TB --- 2013-06-18 01:50:36 - cd /src/sys/arm/conf TB --- 2013-06-18 01:50:36 - /usr/sbin/config -m LINT TB --- 2013-06-18 01:50:36 - building LINT kernel TB --- 2013-06-18 01:50:36 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 01:50:36 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 01:50:36 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 01:50:36 - SRCCONF=/dev/null TB --- 2013-06-18 01:50:36 - TARGET=arm TB --- 2013-06-18 01:50:36 - TARGET_ARCH=arm TB --- 2013-06-18 01:50:36 - TZ=UTC TB --- 2013-06-18 01:50:36 - __MAKE_CONF=/dev/null TB --- 2013-06-18 01:50:36 - cd /src TB --- 2013-06-18 01:50:36 - /usr/bin/make -B buildkernel KERNCONF=LINT >>> Kernel build for LINT started on Tue Jun 18 01:50:36 UTC 2013 >>> stage 1: configuring the kernel >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3.1: making dependencies >>> stage 3.2: building everything >>> Kernel build for LINT completed on Tue Jun 18 02:13:19 UTC 2013 TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m AC100 TB --- 2013-06-18 02:13:19 - skipping AC100 kernel TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m ARMADAXP TB --- 2013-06-18 02:13:19 - skipping ARMADAXP kernel TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m ATMEL TB --- 2013-06-18 02:13:19 - building ATMEL kernel TB --- 2013-06-18 02:13:19 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 02:13:19 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 02:13:19 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 02:13:19 - SRCCONF=/dev/null TB --- 2013-06-18 02:13:19 - TARGET=arm TB --- 2013-06-18 02:13:19 - TARGET_ARCH=arm TB --- 2013-06-18 02:13:19 - TZ=UTC TB --- 2013-06-18 02:13:19 - __MAKE_CONF=/dev/null TB --- 2013-06-18 02:13:19 - cd /src TB --- 2013-06-18 02:13:19 - /usr/bin/make -B buildkernel KERNCONF=ATMEL >>> Kernel build for ATMEL started on Tue Jun 18 02:13:20 UTC 2013 >>> stage 1: configuring the kernel >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3.1: making dependencies >>> stage 3.2: building everything >>> Kernel build for ATMEL completed on Tue Jun 18 02:17:02 UTC 2013 TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m AVILA TB --- 2013-06-18 02:17:02 - skipping AVILA kernel TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m BEAGLEBONE TB --- 2013-06-18 02:17:02 - skipping BEAGLEBONE kernel TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m BWCT TB --- 2013-06-18 02:17:02 - building BWCT kernel TB --- 2013-06-18 02:17:02 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 02:17:02 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 02:17:02 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 02:17:02 - SRCCONF=/dev/null TB --- 2013-06-18 02:17:02 - TARGET=arm TB --- 2013-06-18 02:17:02 - TARGET_ARCH=arm TB --- 2013-06-18 02:17:02 - TZ=UTC TB --- 2013-06-18 02:17:02 - __MAKE_CONF=/dev/null TB --- 2013-06-18 02:17:02 - cd /src TB --- 2013-06-18 02:17:02 - /usr/bin/make -B buildkernel KERNCONF=BWCT >>> Kernel build for BWCT started on Tue Jun 18 02:17:02 UTC 2013 >>> stage 1: configuring the kernel >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3.1: making dependencies >>> stage 3.2: building everything >>> Kernel build for BWCT completed on Tue Jun 18 02:19:35 UTC 2013 TB --- 2013-06-18 02:19:35 - cd /src/sys/arm/conf TB --- 2013-06-18 02:19:35 - /usr/sbin/config -m CAMBRIA TB --- 2013-06-18 02:19:35 - skipping CAMBRIA kernel TB --- 2013-06-18 02:19:35 - cd /src/sys/arm/conf TB --- 2013-06-18 02:19:35 - /usr/sbin/config -m CNS11XXNAS TB --- 2013-06-18 02:19:35 - building CNS11XXNAS kernel TB --- 2013-06-18 02:19:35 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 02:19:35 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 02:19:35 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 02:19:35 - SRCCONF=/dev/null TB --- 2013-06-18 02:19:35 - TARGET=arm TB --- 2013-06-18 02:19:35 - TARGET_ARCH=arm TB --- 2013-06-18 02:19:35 - TZ=UTC TB --- 2013-06-18 02:19:35 - __MAKE_CONF=/dev/null TB --- 2013-06-18 02:19:35 - cd /src TB --- 2013-06-18 02:19:35 - /usr/bin/make -B buildkernel KERNCONF=CNS11XXNAS >>> Kernel build for CNS11XXNAS started on Tue Jun 18 02:19:35 UTC 2013 >>> stage 1: configuring the kernel >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3.1: making dependencies >>> stage 3.2: building everything >>> Kernel build for CNS11XXNAS completed on Tue Jun 18 02:23:05 UTC 2013 TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m CRB TB --- 2013-06-18 02:23:05 - skipping CRB kernel TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m CUBIEBOARD TB --- 2013-06-18 02:23:05 - skipping CUBIEBOARD kernel TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m DB-78XXX TB --- 2013-06-18 02:23:05 - building DB-78XXX kernel TB --- 2013-06-18 02:23:05 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 02:23:05 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 02:23:05 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 02:23:05 - SRCCONF=/dev/null TB --- 2013-06-18 02:23:05 - TARGET=arm TB --- 2013-06-18 02:23:05 - TARGET_ARCH=arm TB --- 2013-06-18 02:23:05 - TZ=UTC TB --- 2013-06-18 02:23:05 - __MAKE_CONF=/dev/null TB --- 2013-06-18 02:23:05 - cd /src TB --- 2013-06-18 02:23:05 - /usr/bin/make -B buildkernel KERNCONF=DB-78XXX >>> Kernel build for DB-78XXX started on Tue Jun 18 02:23:05 UTC 2013 >>> stage 1: configuring the kernel >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3.1: making dependencies -------------------------------------------------------------- cd /obj/arm.arm/src/sys/DB-78XXX; MAKEOBJDIRPREFIX=/obj/arm.arm MACHINE_ARCH=arm MACHINE=arm CPUTYPE= GROFF_BIN_PATH=/obj/arm.arm/src/tmp/legacy/usr/bin GROFF_FONT_PATH=/obj/arm.arm/src/tmp/legacy/usr/share/groff_font GROFF_TMAC_PATH=/obj/arm.arm/src/tmp/legacy/usr/share/tmac _SHLIBDIRPREFIX=/obj/arm.arm/src/tmp _LDSCRIPTROOT= VERSION="FreeBSD 8.3-PRERELEASE amd64 803500" INSTALL="sh /src/tools/install.sh" PATH=/obj/arm.arm/src/tmp/legacy/usr/sbin:/obj/arm.arm/src/tmp/legacy/usr/bin:/obj/arm.arm/src/tmp/legacy/usr/games:/obj/arm.arm/src/tmp/legacy/bin:/obj/arm.arm/src/tmp/usr/sbin:/obj/arm.arm/src/tmp/usr/bin:/obj/arm.arm/src/tmp/usr/games:/sbin:/bin:/usr/sbin:/usr/bin CC="cc " CXX="c++ " CPP="cpp " AS="as" AR="ar" LD="ld" NM=nm OBJDUMP= RANLIB=ranlib STRINGS= COMPILER_TYPE=clang /obj/src/make.amd64/make -B -m /src/share/mk KERNEL=kernel depend -DNO_MODULES_OBJ machine -> /src/sys/arm/include cc -c -O2 -pipe -fno-strict-aliasing -std=c99 -Wall -Wredundant-decls -Wnested-externs -Wstrict-prototypes -Wmissing-prototypes -Wpointer-arith -Winline -Wcast-qual -Wundef -Wno-pointer-sign -fformat-extensions -Wmissing-include-dirs -fdiagnostics-show-option -Wno-error-tautological-compare -Wno-error-empty-body -Wno-error-parentheses-equality -nostdinc -I. -I/src/sys -I/src/sys/contrib/altq -I/src/sys/contrib/ipfilter -I/src/sys/dev/ath -I/src/sys/dev/ath/ath_hal -I/src/sys/contrib/dev/ath/ath_hal -I/src/sys/contrib/ngatm -I/src/sys/dev/twa -I/src/sys/dev/cxgb -I/src/sys/dev/cxgbe -I/src/sys/contrib/libfdt -D_KERNEL -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -march=armv5te -ffreestanding /src/sys/arm/arm/genassym.c NM='nm' sh /src/sys/kern/genassym.sh genassym.o > assym.s awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -p awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -q awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -h if [ -f /src/sys/boot/fdt/dts/db78100.dts ]; then dtc -O dtb -o db78100.dtb -b 0 -p 1024 /src/sys/boot/fdt/dts/db78100.dts; fi *** Signal 11 Stop. make: stopped in /obj/arm.arm/src/sys/DB-78XXX *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-18 02:23:09 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-18 02:23:09 - ERROR: failed to build DB-78XXX kernel TB --- 2013-06-18 02:23:09 - 10061.17 user 1864.69 system 12771.65 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 03:23:23 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id BE22AF40 for ; Tue, 18 Jun 2013 03:23:23 +0000 (UTC) (envelope-from imp@bsdimp.com) Received: from mail-pd0-f175.google.com (mail-pd0-f175.google.com [209.85.192.175]) by mx1.freebsd.org (Postfix) with ESMTP id 9997E12F1 for ; Tue, 18 Jun 2013 03:23:23 +0000 (UTC) Received: by mail-pd0-f175.google.com with SMTP id 4so3416112pdd.6 for ; Mon, 17 Jun 2013 20:23:23 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=sender:subject:mime-version:content-type:from:in-reply-to:date:cc :content-transfer-encoding:message-id:references:to:x-mailer :x-gm-message-state; bh=RUL9tVOVIKXSgvUe4J7q5a0WXRaNGJL7buVAj4XlfFQ=; b=i5woxpfGPUfEu9UvWPzQoYhtWUJYkPLcZN0h8DSGxKDKsmURonmYdGlOdIgr/tfLaL rsEwYGTWGOKMbPCttH3/k9Mful4YeptgvZvCc5IhP1D/rIWjrZi8F6Z6UPqlWRPCpTl3 J+FYdcC8CBrXXjNJ5+8Mgec3i4zmtyn5iPht8wPIXjbOJh4GNKSM9RascoTuJBW7PQfM z48ovNaN72CP0IY7FBBYKc5CNzr4yLD4orq7oXTWx0c3Vc7nnhiZvWL3CQizotX9SQVm KLB35/PXAOtZyCul4aaWWpImLCMefXmssrqqmp9Fis0hP1H3dIchTRpNvuEdgoyJ+xgQ Zwrw== X-Received: by 10.68.189.233 with SMTP id gl9mr11270739pbc.213.1371525802982; Mon, 17 Jun 2013 20:23:22 -0700 (PDT) Received: from 53.imp.bsdimp.com (50-78-194-198-static.hfc.comcastbusiness.net. [50.78.194.198]) by mx.google.com with ESMTPSA id dj5sm6911982pbc.25.2013.06.17.20.23.20 for (version=TLSv1 cipher=ECDHE-RSA-RC4-SHA bits=128/128); Mon, 17 Jun 2013 20:23:21 -0700 (PDT) Sender: Warner Losh Subject: Re: Two questions on -current... Mime-Version: 1.0 (Apple Message framework v1085) Content-Type: text/plain; charset=us-ascii From: Warner Losh In-Reply-To: <1371521474.1391.9.camel@fbsd-laptop> Date: Mon, 17 Jun 2013 21:23:19 -0600 Content-Transfer-Encoding: quoted-printable Message-Id: References: <1371521474.1391.9.camel@fbsd-laptop> To: mcgovern@beta.com X-Mailer: Apple Mail (2.1085) X-Gm-Message-State: ALoCoQnSxF8PlScdgkuPn4YFGF+LZyMg5JqNXFVJWk/2Tr4kwK4qTBKEnGjQTHQwECWx0BZbCuOv Cc: freebsd-arm@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 03:23:23 -0000 On Jun 17, 2013, at 8:11 PM, Brian J. McGovern wrote: > I'm currently using a fairly recent (within the week) -current on a > Beaglebone Black and trying to use it on an OpenRD ultimate... I have > two questions that I can't seem to find recent answers online. >=20 > 1.) On the Beaglebone black, is there an interface for setting up the > MUX on the GPIO pins? I've seen gpioctl, which doesn't seem to have = the > capability, and there seems to be settings in the DTS file, although = it > appears incomplete (e.g. not all pins are configured), but is there a > way to dynamically set up the MUX during run time? There's only limited support for this on some ports. It is one of the = biggest holes we have today. > 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: > unknown target CPU 'armv5te', despite a find ... grep... on the code > showing this option in both gcc and clang compilers and tools. Is this > processor deprecated in current? Is there are a replacement? Did I = miss > a change in how to build the kernel (Currently using "make TARGET=3Darm > TARGET_ARCH=3Darm KERNCONF=3DDB-88F6XXX buildkernel" in /usr/src)? Do you have TARGET_CPU set somewhere? Warner From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 04:10:19 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 308443BD for ; Tue, 18 Jun 2013 04:10:19 +0000 (UTC) (envelope-from jbirch@jbirch.net) Received: from mail-ob0-x231.google.com (mail-ob0-x231.google.com [IPv6:2607:f8b0:4003:c01::231]) by mx1.freebsd.org (Postfix) with ESMTP id F327E16E5 for ; Tue, 18 Jun 2013 04:10:18 +0000 (UTC) Received: by mail-ob0-f177.google.com with SMTP id ta17so4126570obb.36 for ; Mon, 17 Jun 2013 21:10:18 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=mime-version:x-originating-ip:in-reply-to:references:date :message-id:subject:from:to:cc:content-type:x-gm-message-state; bh=VorYQsvI/swC2R7Cdb9WHGto6Rirq72OQBm6N5nq4Ys=; b=okDEcnKZTbRnqL8h/cgVM6QjYOPel+YXox6ZX2EEnaxY7fMHkchNKRfT6JalwYTmfu tEIUcO2S4nhBFC/WE8K2btKdG3QH50Hm7ix7XDccCDkOVH7++1QbSVHlSUB+GCNG59L1 mqY2RAIYJ8kYSQbDILdppigt/2KiXZ0fC11IM0CQUuzeaEbtkVtI6oPpb/Qof7bXTZY6 XYja6CnE7GXaqrMvraqvbkhhs7fCirhPvHIZRfC3EBq0vEQ+znXw2AjR6MPBe3qFfYXT 6WUvWRxT55bcc6N2uMYf68FiWG7P43i5oTERMmJBiWlQGE8Afxe6YDL5iJLRvHwvXADZ zeVA== MIME-Version: 1.0 X-Received: by 10.60.137.163 with SMTP id qj3mr11156556oeb.84.1371528618488; Mon, 17 Jun 2013 21:10:18 -0700 (PDT) Received: by 10.182.216.40 with HTTP; Mon, 17 Jun 2013 21:10:18 -0700 (PDT) X-Originating-IP: [59.167.133.100] In-Reply-To: References: <1371521474.1391.9.camel@fbsd-laptop> Date: Tue, 18 Jun 2013 14:10:18 +1000 Message-ID: Subject: Re: Two questions on -current... From: Jason Birch To: Warner Losh X-Gm-Message-State: ALoCoQl5GQ9K/HM7HUQUP4veNEjyX7AFANCfmW5CiD6ahWdI3YVRLmeam3c1YmTbNzOZ2jjhvoXt Content-Type: text/plain; charset=ISO-8859-1 X-Content-Filtered-By: Mailman/MimeDel 2.1.14 Cc: mcgovern@beta.com, freebsd-arm X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 04:10:19 -0000 > 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: > unknown target CPU 'armv5te', despite a find ... grep... on the code > showing this option in both gcc and clang compilers and tools. Is this > processor deprecated in current? Is there are a replacement? Did I miss > a change in how to build the kernel (Currently using "make TARGET=arm > TARGET_ARCH=arm KERNCONF=DB-88F6XXX buildkernel" in /usr/src)? > You'll need TARGET_ARCH=armv6, I think. From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 04:23:52 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id C2D157EE for ; Tue, 18 Jun 2013 04:23:52 +0000 (UTC) (envelope-from imp@bsdimp.com) Received: from mail-ie0-x234.google.com (mail-ie0-x234.google.com [IPv6:2607:f8b0:4001:c03::234]) by mx1.freebsd.org (Postfix) with ESMTP id 949F4174D for ; Tue, 18 Jun 2013 04:23:52 +0000 (UTC) Received: by mail-ie0-f180.google.com with SMTP id f4so9038702iea.11 for ; Mon, 17 Jun 2013 21:23:52 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=sender:subject:mime-version:content-type:from:in-reply-to:date:cc :content-transfer-encoding:message-id:references:to:x-mailer :x-gm-message-state; bh=6InM8z2DUJxqubljRX/wfQ4MrotMjfe82yWHqQyxsNo=; b=XWbQCMmugH9tbq2NIcwLhrG3B7dGwoPBSkt1El1IpktB089UnWTjrctuqygPyVSbl3 H4oPp23r8BpqT1dRXX5Hex+694R1iX370J1KrJJnZ6QALkiISi5XJJ9nUox3XUhpEFE+ xuoLP/bsKLqBIcqg604bEYsoxs+FYzsyZeu8bpgpPoNYGOrulYZeUNm9K7h93s9q5bsK FT12zF0aUKsBvEadLjPvV+FYc4evKwFqxbRzCg2R85ajvSO8Zr0hE+jyeyX2z7zbxafQ MMmVSCkNnip7+WbC0/4dYV0uG9i756Ltn9Yr0Bhh1m/TIW1KKOJm7uS9OmHCxKyUEdqE K/5g== X-Received: by 10.50.25.194 with SMTP id e2mr6597264igg.111.1371529432307; Mon, 17 Jun 2013 21:23:52 -0700 (PDT) Received: from 53.imp.bsdimp.com (50-78-194-198-static.hfc.comcastbusiness.net. [50.78.194.198]) by mx.google.com with ESMTPSA id ct8sm20555569igb.7.2013.06.17.21.23.50 for (version=TLSv1 cipher=ECDHE-RSA-RC4-SHA bits=128/128); Mon, 17 Jun 2013 21:23:51 -0700 (PDT) Sender: Warner Losh Subject: Re: Two questions on -current... Mime-Version: 1.0 (Apple Message framework v1085) Content-Type: text/plain; charset=us-ascii From: Warner Losh In-Reply-To: Date: Mon, 17 Jun 2013 22:23:49 -0600 Content-Transfer-Encoding: quoted-printable Message-Id: <25ACCE84-5498-43EC-AD9D-D0CC17A8DB65@bsdimp.com> References: <1371521474.1391.9.camel@fbsd-laptop> To: Jason Birch X-Mailer: Apple Mail (2.1085) X-Gm-Message-State: ALoCoQkwfNyCkFXaKfRwUY2FaCQZyvRoN8u+tJOY+G0MnMxRwjFy0McNZGtagRhFgMAIXTyAv7p8 Cc: mcgovern@beta.com, freebsd-arm X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 04:23:52 -0000 On Jun 17, 2013, at 10:10 PM, Jason Birch wrote: > 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: > unknown target CPU 'armv5te', despite a find ... grep... on the code > showing this option in both gcc and clang compilers and tools. Is this > processor deprecated in current? Is there are a replacement? Did I = miss > a change in how to build the kernel (Currently using "make TARGET=3Darm > TARGET_ARCH=3Darm KERNCONF=3DDB-88F6XXX buildkernel" in /usr/src)? >=20 > You'll need TARGET_ARCH=3Darmv6, I think.=20 The Marvel Kirkwood are armv5te. I think the actual problem may be that no buildworld and/or = kernel-toolchain was done first... Warner From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 07:25:33 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 7D3669CF for ; Tue, 18 Jun 2013 07:25:33 +0000 (UTC) (envelope-from alie@affle.com) Received: from mail-qc0-x22b.google.com (mail-qc0-x22b.google.com [IPv6:2607:f8b0:400d:c01::22b]) by mx1.freebsd.org (Postfix) with ESMTP id 2E90F1D87 for ; Tue, 18 Jun 2013 07:25:33 +0000 (UTC) Received: by mail-qc0-f171.google.com with SMTP id n1so2138466qcw.30 for ; Tue, 18 Jun 2013 00:25:32 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type:x-gm-message-state; bh=w+mU2BItu+oO1YubysCjsi4JYxsxtjAKI788UOXaDUo=; b=FN9qURYncosrPBcM+hM3EUpfhDdp8EkbtGBR50jffKopOBlsZDpayen89umVwjPeh2 zZkAETQl8QyEsTpMsvNDunD+5TxF9LECB4Adsz3OOjcYqybmBRTGz50jCOHCI5u7wYRR BaBOf8QTcph4YdfknTcgnEZ4ncDs8y3SDHYLjZDQOcWJq41ci78Vx4pud6kz/RXxdidH 8FkzdQc7vaUgT26Nh/9gzkHjC1gbN3P9JBnX7etiiPxD3mX2B3LmOCmf+qt9HH7nZHpm +wmZTvY4Nx+rBVXdyQVkNOUPi67eGJ34s/PKu8XSPIO25nWNOwOMg5S/bCYJwJux5XOW Ai+w== MIME-Version: 1.0 X-Received: by 10.49.62.33 with SMTP id v1mr25652609qer.53.1371540332602; Tue, 18 Jun 2013 00:25:32 -0700 (PDT) Received: by 10.49.84.168 with HTTP; Tue, 18 Jun 2013 00:25:32 -0700 (PDT) In-Reply-To: <201306180223.r5I2N9S9040413@freebsd-current.sentex.ca> References: <201306180223.r5I2N9S9040413@freebsd-current.sentex.ca> Date: Tue, 18 Jun 2013 15:25:32 +0800 Message-ID: Subject: Re: [head tinderbox] failure on arm/arm From: Alie Tan To: FreeBSD Tinderbox X-Gm-Message-State: ALoCoQmcrEGvdjVWluM3A8me2EROE5U7+r7k5+VbyLjjfEOK8PiQfLluDqg8hdGkFmfEiOY54Tqe Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable X-Content-Filtered-By: Mailman/MimeDel 2.1.14 Cc: "freebsd-arm@freebsd.org" , current@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 07:25:33 -0000 This revision causing the issue http://freshbsd.org/commit/freebsd/r251856 I have to revert the revision to solve the issue On Tue, Jun 18, 2013 at 10:23 AM, FreeBSD Tinderbox wrote: > TB --- 2013-06-17 22:50:17 - tinderbox 2.10 running on > freebsd-current.sentex.ca > TB --- 2013-06-17 22:50:17 - FreeBSD freebsd-current.sentex.ca8.3-PRERELE= ASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 > des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 > TB --- 2013-06-17 22:50:17 - starting HEAD tinderbox run for arm/arm > TB --- 2013-06-17 22:50:17 - cleaning the object tree > TB --- 2013-06-17 22:50:17 - /usr/local/bin/svn stat /src > TB --- 2013-06-17 22:50:22 - At svn revision 251871 > TB --- 2013-06-17 22:50:23 - building world > TB --- 2013-06-17 22:50:23 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-17 22:50:23 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-17 22:50:23 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-17 22:50:23 - SRCCONF=3D/dev/null > TB --- 2013-06-17 22:50:23 - TARGET=3Darm > TB --- 2013-06-17 22:50:23 - TARGET_ARCH=3Darm > TB --- 2013-06-17 22:50:23 - TZ=3DUTC > TB --- 2013-06-17 22:50:23 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-17 22:50:23 - cd /src > TB --- 2013-06-17 22:50:23 - /usr/bin/make -B buildworld > >>> Building an up-to-date make(1) > >>> World build started on Mon Jun 17 22:50:29 UTC 2013 > >>> Rebuilding the temporary build tree > >>> stage 1.1: legacy release compatibility shims > >>> stage 1.2: bootstrap tools > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3: cross tools > >>> stage 4.1: building includes > >>> stage 4.2: building libraries > >>> stage 4.3: make dependencies > >>> stage 4.4: building everything > >>> World build completed on Tue Jun 18 01:50:36 UTC 2013 > TB --- 2013-06-18 01:50:36 - generating LINT kernel config > TB --- 2013-06-18 01:50:36 - cd /src/sys/arm/conf > TB --- 2013-06-18 01:50:36 - /usr/bin/make -B LINT > TB --- 2013-06-18 01:50:36 - cd /src/sys/arm/conf > TB --- 2013-06-18 01:50:36 - /usr/sbin/config -m LINT > TB --- 2013-06-18 01:50:36 - building LINT kernel > TB --- 2013-06-18 01:50:36 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-18 01:50:36 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-18 01:50:36 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-18 01:50:36 - SRCCONF=3D/dev/null > TB --- 2013-06-18 01:50:36 - TARGET=3Darm > TB --- 2013-06-18 01:50:36 - TARGET_ARCH=3Darm > TB --- 2013-06-18 01:50:36 - TZ=3DUTC > TB --- 2013-06-18 01:50:36 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-18 01:50:36 - cd /src > TB --- 2013-06-18 01:50:36 - /usr/bin/make -B buildkernel KERNCONF=3DLINT > >>> Kernel build for LINT started on Tue Jun 18 01:50:36 UTC 2013 > >>> stage 1: configuring the kernel > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3.1: making dependencies > >>> stage 3.2: building everything > >>> Kernel build for LINT completed on Tue Jun 18 02:13:19 UTC 2013 > TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m AC100 > TB --- 2013-06-18 02:13:19 - skipping AC100 kernel > TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m ARMADAXP > TB --- 2013-06-18 02:13:19 - skipping ARMADAXP kernel > TB --- 2013-06-18 02:13:19 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:13:19 - /usr/sbin/config -m ATMEL > TB --- 2013-06-18 02:13:19 - building ATMEL kernel > TB --- 2013-06-18 02:13:19 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-18 02:13:19 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-18 02:13:19 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-18 02:13:19 - SRCCONF=3D/dev/null > TB --- 2013-06-18 02:13:19 - TARGET=3Darm > TB --- 2013-06-18 02:13:19 - TARGET_ARCH=3Darm > TB --- 2013-06-18 02:13:19 - TZ=3DUTC > TB --- 2013-06-18 02:13:19 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-18 02:13:19 - cd /src > TB --- 2013-06-18 02:13:19 - /usr/bin/make -B buildkernel KERNCONF=3DATME= L > >>> Kernel build for ATMEL started on Tue Jun 18 02:13:20 UTC 2013 > >>> stage 1: configuring the kernel > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3.1: making dependencies > >>> stage 3.2: building everything > >>> Kernel build for ATMEL completed on Tue Jun 18 02:17:02 UTC 2013 > TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m AVILA > TB --- 2013-06-18 02:17:02 - skipping AVILA kernel > TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m BEAGLEBONE > TB --- 2013-06-18 02:17:02 - skipping BEAGLEBONE kernel > TB --- 2013-06-18 02:17:02 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:17:02 - /usr/sbin/config -m BWCT > TB --- 2013-06-18 02:17:02 - building BWCT kernel > TB --- 2013-06-18 02:17:02 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-18 02:17:02 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-18 02:17:02 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-18 02:17:02 - SRCCONF=3D/dev/null > TB --- 2013-06-18 02:17:02 - TARGET=3Darm > TB --- 2013-06-18 02:17:02 - TARGET_ARCH=3Darm > TB --- 2013-06-18 02:17:02 - TZ=3DUTC > TB --- 2013-06-18 02:17:02 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-18 02:17:02 - cd /src > TB --- 2013-06-18 02:17:02 - /usr/bin/make -B buildkernel KERNCONF=3DBWCT > >>> Kernel build for BWCT started on Tue Jun 18 02:17:02 UTC 2013 > >>> stage 1: configuring the kernel > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3.1: making dependencies > >>> stage 3.2: building everything > >>> Kernel build for BWCT completed on Tue Jun 18 02:19:35 UTC 2013 > TB --- 2013-06-18 02:19:35 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:19:35 - /usr/sbin/config -m CAMBRIA > TB --- 2013-06-18 02:19:35 - skipping CAMBRIA kernel > TB --- 2013-06-18 02:19:35 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:19:35 - /usr/sbin/config -m CNS11XXNAS > TB --- 2013-06-18 02:19:35 - building CNS11XXNAS kernel > TB --- 2013-06-18 02:19:35 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-18 02:19:35 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-18 02:19:35 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-18 02:19:35 - SRCCONF=3D/dev/null > TB --- 2013-06-18 02:19:35 - TARGET=3Darm > TB --- 2013-06-18 02:19:35 - TARGET_ARCH=3Darm > TB --- 2013-06-18 02:19:35 - TZ=3DUTC > TB --- 2013-06-18 02:19:35 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-18 02:19:35 - cd /src > TB --- 2013-06-18 02:19:35 - /usr/bin/make -B buildkernel > KERNCONF=3DCNS11XXNAS > >>> Kernel build for CNS11XXNAS started on Tue Jun 18 02:19:35 UTC 2013 > >>> stage 1: configuring the kernel > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3.1: making dependencies > >>> stage 3.2: building everything > >>> Kernel build for CNS11XXNAS completed on Tue Jun 18 02:23:05 UTC 2013 > TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m CRB > TB --- 2013-06-18 02:23:05 - skipping CRB kernel > TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m CUBIEBOARD > TB --- 2013-06-18 02:23:05 - skipping CUBIEBOARD kernel > TB --- 2013-06-18 02:23:05 - cd /src/sys/arm/conf > TB --- 2013-06-18 02:23:05 - /usr/sbin/config -m DB-78XXX > TB --- 2013-06-18 02:23:05 - building DB-78XXX kernel > TB --- 2013-06-18 02:23:05 - CROSS_BUILD_TESTING=3DYES > TB --- 2013-06-18 02:23:05 - MAKEOBJDIRPREFIX=3D/obj > TB --- 2013-06-18 02:23:05 - PATH=3D/usr/bin:/usr/sbin:/bin:/sbin > TB --- 2013-06-18 02:23:05 - SRCCONF=3D/dev/null > TB --- 2013-06-18 02:23:05 - TARGET=3Darm > TB --- 2013-06-18 02:23:05 - TARGET_ARCH=3Darm > TB --- 2013-06-18 02:23:05 - TZ=3DUTC > TB --- 2013-06-18 02:23:05 - __MAKE_CONF=3D/dev/null > TB --- 2013-06-18 02:23:05 - cd /src > TB --- 2013-06-18 02:23:05 - /usr/bin/make -B buildkernel KERNCONF=3DDB-7= 8XXX > >>> Kernel build for DB-78XXX started on Tue Jun 18 02:23:05 UTC 2013 > >>> stage 1: configuring the kernel > >>> stage 2.1: cleaning up the object tree > >>> stage 2.2: rebuilding the object tree > >>> stage 2.3: build tools > >>> stage 3.1: making dependencies > -------------------------------------------------------------- > cd /obj/arm.arm/src/sys/DB-78XXX; MAKEOBJDIRPREFIX=3D/obj/arm.arm > MACHINE_ARCH=3Darm MACHINE=3Darm CPUTYPE=3D > GROFF_BIN_PATH=3D/obj/arm.arm/src/tmp/legacy/usr/bin > GROFF_FONT_PATH=3D/obj/arm.arm/src/tmp/legacy/usr/share/groff_font > GROFF_TMAC_PATH=3D/obj/arm.arm/src/tmp/legacy/usr/share/tmac > _SHLIBDIRPREFIX=3D/obj/arm.arm/src/tmp _LDSCRIPTROOT=3D VERSION=3D"Fre= eBSD > 8.3-PRERELEASE amd64 803500" INSTALL=3D"sh /src/tools/install.sh" > PATH=3D/obj/arm.arm/src/tmp/legacy/usr/sbin:/obj/arm.arm/src/tmp/legacy/= usr/bin:/obj/arm.arm/src/tmp/legacy/usr/games:/obj/arm.arm/src/tmp/legacy/b= in:/obj/arm.arm/src/tmp/usr/sbin:/obj/arm.arm/src/tmp/usr/bin:/obj/arm.arm/= src/tmp/usr/games:/sbin:/bin:/usr/sbin:/usr/bin > CC=3D"cc " CXX=3D"c++ " CPP=3D"cpp " AS=3D"as" AR=3D"ar" LD=3D"ld" NM= =3Dnm OBJDUMP=3D > RANLIB=3Dranlib STRINGS=3D COMPILER_TYPE=3Dclang /obj/src/make.amd64/make= -B -m > /src/share/mk KERNEL=3Dkernel depend -DNO_MODULES_OBJ > machine -> /src/sys/arm/include > cc -c -O2 -pipe -fno-strict-aliasing -std=3Dc99 -Wall -Wredundant-decls > -Wnested-externs -Wstrict-prototypes -Wmissing-prototypes -Wpointer-arith > -Winline -Wcast-qual -Wundef -Wno-pointer-sign -fformat-extensions > -Wmissing-include-dirs -fdiagnostics-show-option > -Wno-error-tautological-compare -Wno-error-empty-body > -Wno-error-parentheses-equality -nostdinc -I. -I/src/sys > -I/src/sys/contrib/altq -I/src/sys/contrib/ipfilter -I/src/sys/dev/ath > -I/src/sys/dev/ath/ath_hal -I/src/sys/contrib/dev/ath/ath_hal > -I/src/sys/contrib/ngatm -I/src/sys/dev/twa -I/src/sys/dev/cxgb > -I/src/sys/dev/cxgbe -I/src/sys/contrib/libfdt -D_KERNEL > -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -march=3Darmv5te > -ffreestanding /src/sys/arm/arm/genassym.c > NM=3D'nm' sh /src/sys/kern/genassym.sh genassym.o > assym.s > awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -p > awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -q > awk -f /src/sys/tools/vnode_if.awk /src/sys/kern/vnode_if.src -h > if [ -f /src/sys/boot/fdt/dts/db78100.dts ]; then dtc -O dtb -o > db78100.dtb -b 0 -p 1024 /src/sys/boot/fdt/dts/db78100.dts; fi > *** Signal 11 > > Stop. > make: stopped in /obj/arm.arm/src/sys/DB-78XXX > *** Error code 1 > > Stop. > make: stopped in /src > *** Error code 1 > > Stop in /src. > TB --- 2013-06-18 02:23:09 - WARNING: /usr/bin/make returned exit code 1 > TB --- 2013-06-18 02:23:09 - ERROR: failed to build DB-78XXX kernel > TB --- 2013-06-18 02:23:09 - 10061.17 user 1864.69 system 12771.65 real > > > http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full > _______________________________________________ > freebsd-arm@freebsd.org mailing list > http://lists.freebsd.org/mailman/listinfo/freebsd-arm > To unsubscribe, send any mail to "freebsd-arm-unsubscribe@freebsd.org" > From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 10:39:09 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id AFB67EFC for ; Tue, 18 Jun 2013 10:39:09 +0000 (UTC) (envelope-from alie@affle.com) Received: from mail-qc0-x235.google.com (mail-qc0-x235.google.com [IPv6:2607:f8b0:400d:c01::235]) by mx1.freebsd.org (Postfix) with ESMTP id 6D6411EC4 for ; Tue, 18 Jun 2013 10:39:09 +0000 (UTC) Received: by mail-qc0-f181.google.com with SMTP id u12so2169424qcx.26 for ; Tue, 18 Jun 2013 03:39:08 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :content-type:x-gm-message-state; bh=PX6LPJ9lQRUeEUnB7IVBvZ14rt/+65m+E7wbIKKkDko=; b=Rp8mYOjZfai9wOiNuKkYoGFpgMTRYv3pIdt2o6sCrRVDSfreKWnmv3wRJ0Ms5Icupb en222Csj5zTBAqKkk2YZ9GeILfx5m+qA2a2MyPgSJ/s8nrYKTyYFEVAaBqdBS/fC7gC8 r0aehF/jeRR1eagtt2fANuojyYXjzuDyH+yLN0Ti6XmqP687uh5//R4cwv/JVnGqZzIj sJ7xqIm9aUhUxLs+Fql52KXP1t/DGNJHPKqmX3LmAORK+eUT2CePJUY7ntEiOHQEXAiy a6yuAsi046TLGdpYWYvyeF8/FOvGvBN/eTEIA1EaX3qwOhODXMcEOBGQVCsdhNxk00d8 O8aQ== MIME-Version: 1.0 X-Received: by 10.224.22.197 with SMTP id o5mr21635234qab.52.1371551948765; Tue, 18 Jun 2013 03:39:08 -0700 (PDT) Received: by 10.49.84.168 with HTTP; Tue, 18 Jun 2013 03:39:08 -0700 (PDT) In-Reply-To: <20130610181256.GC81276@funkthat.com> References: <20130605084224.67c84c15@bender.Home> <51B5D6B4.6060902@gmx.de> <20130610181256.GC81276@funkthat.com> Date: Tue, 18 Jun 2013 18:39:08 +0800 Message-ID: Subject: Re: Unable to build 10-CURRENT for Raspi From: Alie Tan To: Jason Birch , Marco Hafke , freebsd-arm X-Gm-Message-State: ALoCoQkEZbobYBro0mzGIFLAKPiEiebdWlPM0NfVPQXk6JncvArBwsPpFSaoQWGbOoXH1MUrsDiw Content-Type: text/plain; charset=ISO-8859-1 X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 10:39:09 -0000 Another compilation issue /usr/src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:500:10: error: duplicate case value '4' case sizeof(apr_int64_t): ^ /usr/src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:498:10: note: previous case defined here case sizeof(apr_int32_t): ^ /usr/src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:671:10: error: duplicate case value '4' case sizeof(apr_int64_t): ^ /usr/src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:669:10: note: previous case defined here case sizeof(apr_int32_t): ^ 2 errors generated. *** Error code 1 Stop. make: stopped in /usr/src/usr.bin/svn/lib/libapr *** Error code 1 Stop. make: stopped in /usr/src/usr.bin/svn/lib *** Error code 1 Stop. make: stopped in /usr/src/usr.bin/svn *** Error code 1 Stop. make: stopped in /usr/src/usr.bin *** Error code 1 Stop. make: stopped in /usr/src *** Error code 1 Stop. make: stopped in /usr/src *** [buildworld] Error code 1 On Tue, Jun 11, 2013 at 2:12 AM, John-Mark Gurney wrote: > Jason Birch wrote this message on Tue, Jun 11, 2013 at 00:09 +1000: > > > I'm currently building for BeagleBone using r251352 (June 3rd), and > > > everything seems okay so far. > > > > > > > Actually, looks like that's crapping out for an unrelated reason. May be > my > > environment or may be that revision, but it might be safest to roll with > > r251213 instead :) > > r251604 fixed the build... > > -- > John-Mark Gurney Voice: +1 415 225 5579 > > "All that I will do, has been done, All that I have, has not." > _______________________________________________ > freebsd-arm@freebsd.org mailing list > http://lists.freebsd.org/mailman/listinfo/freebsd-arm > To unsubscribe, send any mail to "freebsd-arm-unsubscribe@freebsd.org" > From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 12:36:41 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id CF33757A; Tue, 18 Jun 2013 12:36:41 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id 81C531740; Tue, 18 Jun 2013 12:36:41 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5ICaeOZ069777; Tue, 18 Jun 2013 08:36:40 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5ICaeIr069776; Tue, 18 Jun 2013 12:36:40 GMT (envelope-from tinderbox@freebsd.org) Date: Tue, 18 Jun 2013 12:36:40 GMT Message-Id: <201306181236.r5ICaeIr069776@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 12:36:41 -0000 TB --- 2013-06-18 09:40:39 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-18 09:40:39 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-18 09:40:39 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-18 09:40:39 - cleaning the object tree TB --- 2013-06-18 09:43:12 - /usr/local/bin/svn stat /src TB --- 2013-06-18 09:43:15 - At svn revision 251925 TB --- 2013-06-18 09:43:16 - building world TB --- 2013-06-18 09:43:16 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 09:43:16 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 09:43:16 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 09:43:16 - SRCCONF=/dev/null TB --- 2013-06-18 09:43:16 - TARGET=arm TB --- 2013-06-18 09:43:16 - TARGET_ARCH=arm TB --- 2013-06-18 09:43:16 - TZ=UTC TB --- 2013-06-18 09:43:16 - __MAKE_CONF=/dev/null TB --- 2013-06-18 09:43:16 - cd /src TB --- 2013-06-18 09:43:16 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Tue Jun 18 09:43:23 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools >>> stage 4.1: building includes >>> stage 4.2: building libraries >>> stage 4.3: make dependencies >>> stage 4.4: building everything [...] ^ /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:671:10: error: duplicate case value '4' case sizeof(apr_int64_t): ^ /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/strings/apr_snprintf.c:669:10: note: previous case defined here case sizeof(apr_int32_t): ^ 2 errors generated. *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib/libapr *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib *** Error code 1 Stop. make: stopped in /src/usr.bin/svn *** Error code 1 Stop. make: stopped in /src/usr.bin *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-18 12:36:40 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-18 12:36:40 - ERROR: failed to build world TB --- 2013-06-18 12:36:40 - 8435.16 user 1421.29 system 10560.70 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 14:10:10 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 65B72552 for ; Tue, 18 Jun 2013 14:10:10 +0000 (UTC) (envelope-from M.Reyelt@Brunel.de) Received: from mailer1.brunel.de (mailer1.brunel.de [57.66.180.133]) by mx1.freebsd.org (Postfix) with ESMTP id 2741F1BDE for ; Tue, 18 Jun 2013 14:10:09 +0000 (UTC) Received: from mailer1.brunel.de (localhost [127.0.0.1]) by localhost (Postfix) with SMTP id 0D4B578019E for ; Tue, 18 Jun 2013 16:01:40 +0200 (CEST) Received: from mail-hv.brunel.de (mail-hv.brunellocal.de [192.168.1.234]) by mailer1.brunel.de (Postfix) with ESMTP id D06E87801A6 for ; Tue, 18 Jun 2013 16:01:39 +0200 (CEST) Subject: Matthias Reyelt is out of office. From: M.Reyelt@Brunel.de To: freebsd-arm@freebsd.org Message-ID: Date: Tue, 18 Jun 2013 16:01:31 +0200 X-MIMETrack: Serialize by Router on HUB10149/Brunel/De(Release 7.0.4FP2|June 06, 2010) at 18.06.2013 04:01:39 PM MIME-Version: 1.0 Content-type: text/plain; charset=ISO-8859-1 Content-transfer-encoding: quoted-printable X-PMX-Version: 6.0.0.2142326, Antispam-Engine: 2.7.2.2107409, Antispam-Data: 2013.6.18.135133 X-Spam-Probability: Probability=8% X-Spam-Hits: HTML_00_01 0.05, HTML_00_10 0.05, BODYTEXTP_SIZE_3000_LESS 0, BODY_SIZE_1000_LESS 0, BODY_SIZE_100_199 0, BODY_SIZE_2000_LESS 0, BODY_SIZE_5000_LESS 0, BODY_SIZE_7000_LESS 0, BOUNCE_AUTORESP 0, BOUNCE_GENERIC 0, NO_REAL_NAME 0, NO_URI_FOUND 0, SMALL_BODY 0, __BOUNCE_AUTORESP_SUBJ 0, __CT 0, __CTE 0, __CT_TEXT_PLAIN 0, __HAS_FROM 0, __HAS_MSGID 0, __MIME_TEXT_ONLY 0, __MIME_VERSION 0, __SANE_MSGID 0, __TO_MALFORMED_2 0, __TO_NO_NAME 0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 14:10:10 -0000 Ich werde ab Di, 06/18/2013 nicht im B=FCro sein. Ich kehre zur=FCck am= Do, 06/20/2013. I will respond to your message when I return on Friday 21. Regards Matthias= From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 19:10:00 2013 Return-Path: Delivered-To: freebsd-arm@smarthost.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id AA01EE3E for ; Tue, 18 Jun 2013 19:10:00 +0000 (UTC) (envelope-from gnats@FreeBSD.org) Received: from freefall.freebsd.org (freefall.freebsd.org [IPv6:2001:1900:2254:206c::16:87]) by mx1.freebsd.org (Postfix) with ESMTP id 8C28A1E43 for ; Tue, 18 Jun 2013 19:10:00 +0000 (UTC) Received: from freefall.freebsd.org (localhost [127.0.0.1]) by freefall.freebsd.org (8.14.7/8.14.7) with ESMTP id r5IJA0MM060899 for ; Tue, 18 Jun 2013 19:10:00 GMT (envelope-from gnats@freefall.freebsd.org) Received: (from gnats@localhost) by freefall.freebsd.org (8.14.7/8.14.7/Submit) id r5IJA0Xu060898; Tue, 18 Jun 2013 19:10:00 GMT (envelope-from gnats) Resent-Date: Tue, 18 Jun 2013 19:10:00 GMT Resent-Message-Id: <201306181910.r5IJA0Xu060898@freefall.freebsd.org> Resent-From: FreeBSD-gnats-submit@FreeBSD.org (GNATS Filer) Resent-To: freebsd-arm@FreeBSD.org Resent-Reply-To: FreeBSD-gnats-submit@FreeBSD.org, Luiz Otavio O Souza Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id E1D8465A for ; Tue, 18 Jun 2013 19:00:00 +0000 (UTC) (envelope-from nobody@FreeBSD.org) Received: from oldred.freebsd.org (oldred.freebsd.org [8.8.178.121]) by mx1.freebsd.org (Postfix) with ESMTP id D4D001D91 for ; Tue, 18 Jun 2013 19:00:00 +0000 (UTC) Received: from oldred.freebsd.org ([127.0.1.6]) by oldred.freebsd.org (8.14.5/8.14.7) with ESMTP id r5IJ003N073337 for ; Tue, 18 Jun 2013 19:00:00 GMT (envelope-from nobody@oldred.freebsd.org) Received: (from nobody@localhost) by oldred.freebsd.org (8.14.5/8.14.5/Submit) id r5IJ004T073335; Tue, 18 Jun 2013 19:00:00 GMT (envelope-from nobody) Message-Id: <201306181900.r5IJ004T073335@oldred.freebsd.org> Date: Tue, 18 Jun 2013 19:00:00 GMT From: Luiz Otavio O Souza To: freebsd-gnats-submit@FreeBSD.org X-Send-Pr-Version: www-3.1 Subject: arm/179688: [patch] [rpi] serial console eats some characters at moutroot prompt X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 19:10:00 -0000 >Number: 179688 >Category: arm >Synopsis: [patch] [rpi] serial console eats some characters at moutroot prompt >Confidential: no >Severity: non-critical >Priority: low >Responsible: freebsd-arm >State: open >Quarter: >Keywords: >Date-Required: >Class: sw-bug >Submitter-Id: current-users >Arrival-Date: Tue Jun 18 19:10:00 UTC 2013 >Closed-Date: >Last-Modified: >Originator: Luiz Otavio O Souza >Release: -head r251700 >Organization: >Environment: FreeBSD raspberry-pi 10.0-CURRENT FreeBSD 10.0-CURRENT #11 r251700M: Tue Jun 18 13:06:54 BRT 2013 root@devel:/data/rpi/rpi/obj/arm.armv6/data/rpi/rpi/src/sys/RPI-B arm >Description: While at mountroot prompt the rpi uart driver eats some characters, making very hard to type something right. ray@ suggested to not enable the uart interrupts in uart_bus_attach() routine for the console device and that seems to also works fine for rpi. >How-To-Repeat: Boot a kernel from BOOTP (or boot a kernel from SD card without a valid root partition) and try to type at mountroot prompt. You need to keep the keys pressed for a while to see some output. >Fix: Apply the attached patch. It is a copy from the workaround used on uart_dev_imx.c. Patch attached with submission follows: Index: dev/uart/uart_dev_pl011.c =================================================================== --- dev/uart/uart_dev_pl011.c (revision 251700) +++ dev/uart/uart_dev_pl011.c (working copy) @@ -273,8 +273,13 @@ struct uart_bas *bas; bas = &sc->sc_bas; - /* Enable RX & TX interrupts */ - __uart_setreg(bas, UART_IMSC, (UART_RXREADY | UART_TXEMPTY)); + /* XXX workaround to have working console on manut prompt */ + if (sc->sc_sysdev != NULL && sc->sc_sysdev->type == UART_DEV_CONSOLE){ + /* Don't enable interrupts */ + } else { + /* Enable RX & TX interrupts */ + __uart_setreg(bas, UART_IMSC, (UART_RXREADY | UART_TXEMPTY)); + } /* Clear RX & TX interrupts */ __uart_setreg(bas, UART_ICR, IMSC_MASK_ALL); >Release-Note: >Audit-Trail: >Unformatted: From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 19:23:25 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 648031AA for ; Tue, 18 Jun 2013 19:23:25 +0000 (UTC) (envelope-from rskanth@yahoo.com) Received: from nm26-vm0.bullet.mail.bf1.yahoo.com (nm26-vm0.bullet.mail.bf1.yahoo.com [98.139.213.74]) by mx1.freebsd.org (Postfix) with ESMTP id EC3391EB3 for ; Tue, 18 Jun 2013 19:23:24 +0000 (UTC) Received: from [98.139.214.32] by nm26.bullet.mail.bf1.yahoo.com with NNFMP; 18 Jun 2013 19:23:24 -0000 Received: from [98.139.211.205] by tm15.bullet.mail.bf1.yahoo.com with NNFMP; 18 Jun 2013 19:23:24 -0000 Received: from [127.0.0.1] by smtp214.mail.bf1.yahoo.com with NNFMP; 18 Jun 2013 19:23:24 -0000 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=yahoo.com; s=s1024; t=1371583404; bh=aaM/DmIT85bLUzFnOrzn2Z8FeoN5uZiZz8+ZAids91Y=; h=X-Yahoo-Newman-Id:X-Yahoo-Newman-Property:X-YMail-OSG:X-Yahoo-SMTP:X-Rocket-Received:Message-ID:Date:From:User-Agent:MIME-Version:To:CC:Subject:References:In-Reply-To:Content-Type; b=meMlDXUllQKXHETF27E9pR0Viqu8+/E/hW6sSR2u+tKUVglW7EdCK3k6i6x4nhXDFZ4erTBrtAPTvS7ELvfFpHUoD6/yr+hHzjZoxgWCfTbjlYQ3+5HNXXAvuRYdlKRmJkiemCJeu3DcVOeWgBh3QYeSjycxa58o2Hrz1ulyZ/g= X-Yahoo-Newman-Id: 26719.5551.bm@smtp214.mail.bf1.yahoo.com X-Yahoo-Newman-Property: ymail-3 X-YMail-OSG: JPpNyVwVM1n7azU0n7Bu5RlnMSfrH3__hqnqQJluWF4Ukkx DWqVYoGNmeafqksxUOeuLvmE28Gr85wgIcjxWSwBMk4NAjOOZBdb0e8PRoud wrxDHhTyjBlQlWIkSecbfS16_FJ.3wsyOBiA_nHvFGcY1FfEflAjwN7z59Gm KwuzKwXSe4sg.cVxzmEpAvoaJSFFqi3cgf4ywdJPUaQ26B4yAx5aXwGixuNn iwfPBFc3tMCcq0RKDQSHeHdrt_s7hEbR.Ef4xd2wByn2V6kmiEQ26FdcwXuu hnAMhd9zrnuXVhhUCgVqDC6BBzWVT40vKQZX8wp.8tXzHEtp75w03.X2ABTm bLCBEqVK9ny8Wrv.dt0ws8tchilNFpt32T9dLvwh6TdIPNkzpTwkiJueb5Af Wj5d_ejhuJVbmlE56IJKhCQ6mktr.aW_whLP_poSB6nimcLr0NxVQoueQQlr OdHhyc80.u0MsDCcGPwjmGalkL7nZhh7xhR62.Ay3J9NkFSyLyDP1AG.ny8r 3D62qS29Il8KKsfB6mQYay86zcCoGaiSxMp3LHWAFgK5hIs_mz1NBR3wagZ1 Z1B.LnZ33dva_oyiWXo3dIhcmgIIrsjq3LlquB4Q- X-Yahoo-SMTP: 0vhBds2swBAUIWerZ77I22nIbgU- X-Rocket-Received: from sreekanth.voilavip.com (rskanth@24.130.110.113 with ) by smtp214.mail.bf1.yahoo.com with SMTP; 18 Jun 2013 12:23:23 -0700 PDT Message-ID: <51C0B3AA.3060304@yahoo.com> Date: Tue, 18 Jun 2013 12:23:22 -0700 From: Sreekanth Rupavatharam User-Agent: Mozilla/5.0 (Macintosh; Intel Mac OS X 10.8; rv:17.0) Gecko/20130509 Thunderbird/17.0.6 MIME-Version: 1.0 To: Andrey Fesenko Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi References: <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> In-Reply-To: Content-Type: text/plain; charset=UTF-8; format=flowed Content-Transfer-Encoding: 7bit X-Content-Filtered-By: Mailman/MimeDel 2.1.14 Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 19:23:25 -0000 On 6/17/13 3:04 PM, Andrey Fesenko wrote: > i'm rebuild devel/pcre > http://armv6.bsdnir.info.ipv4.sixxs.org/files/pcre_build.log > > are you build image on the system with blank /etc/make.conf? may be > you build clang version > # gcc -v > Using built-in specs. > Target: armv6-undermydesk-freebsd > Configured with: FreeBSD/armv6 system compiler > Thread model: posix > gcc version 4.2.1 20070831 patched [FreeBSD] > # g++ -v > Using built-in specs. > Target: armv6-undermydesk-freebsd > Configured with: FreeBSD/armv6 system compiler > Thread model: posix > gcc version 4.2.1 20070831 patched [FreeBSD] > > or you RPi have /etc/make.conf with clang I tried with clang and g++ with same error. Can you share your /etc/make.conf? From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 21:03:36 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id B0EDF160 for ; Tue, 18 Jun 2013 21:03:36 +0000 (UTC) (envelope-from mercanoles@gmail.com) Received: from mail-pb0-x22e.google.com (mail-pb0-x22e.google.com [IPv6:2607:f8b0:400e:c01::22e]) by mx1.freebsd.org (Postfix) with ESMTP id 92C461301 for ; Tue, 18 Jun 2013 21:03:36 +0000 (UTC) Received: by mail-pb0-f46.google.com with SMTP id rq2so4305749pbb.19 for ; Tue, 18 Jun 2013 14:03:36 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:date:message-id:subject:from:to:content-type; bh=wnw5EflT3I2ii2BEVFcTJ/6/jpJg54Y2FWCycCZON8E=; b=O6ul5aNflf8QbUzq32yo03mmjEyN7zF5ngtEuzb/g+MzEWOGE/DMRYrXsfwHgprlsC cs0i0BuBv665C+xwbzNdme4FFYC/et4wLqrL32eh713L5iDG8OIwSWt/4jZsxMuDQzB7 LbRDkfTG3RZGEj8/MiPHgwrprIgTrww26F4F8FptCXizRSQckjCooigVJY6G+9XkzAZP nszlWcfDp7A1Ot9WWYC7M1Byqfmzoi+nqMdjIvXfizKTZz6ouI8vJOMk+QMuw0AraFHF JDJBrmeFxAz1FPXJ7VkkkwUSwvr306alcXTECNOtjGaJNLyDgmFmkho7xUOwF8+LXMxB aIwg== MIME-Version: 1.0 X-Received: by 10.68.211.73 with SMTP id na9mr18865669pbc.90.1371589416440; Tue, 18 Jun 2013 14:03:36 -0700 (PDT) Received: by 10.70.83.33 with HTTP; Tue, 18 Jun 2013 14:03:36 -0700 (PDT) Date: Tue, 18 Jun 2013 18:03:36 -0300 Message-ID: Subject: Booting problem on mele_a1000(Alwinner A10) From: Mariano Lescano To: freebsd-arm@freebsd.org Content-Type: text/plain; charset=ISO-8859-1 X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 21:03:36 -0000 Hi! We are trying to run FreeBSD on mele_a1000(Allwiner a10). At this moment we have running u-boot-sunxi-current with ethernet support and compiled it with API and ELF support. Also ubldr runs correctly, we can explore the file system and run all the commands and kernel is loaded in memory. When we try to boot the kernel, the boot process stops before printing the copyright output. This is the console output we have: ========================================================== ## Starting application at 0x48000054 ... Consoles: U-Boot console Compatible API signature found @5fe68100 Number of U-Boot devices: 2 FreeBSD/armv6 U-Boot loader, Revision 1.2 (root@mcvlab1, Fri Jun 7 16:34:55 ART 2013) DRAM: 512MB Device: disk - /boot/kernel/kernel data=0x3862a4+0x17b004 syms=[0x4+0x6aed0+0x4+0x44d7e] Hit [Enter] to boot immediately, or any other key for command prompt. Booting [/boot/kernel/kernel]... Using DTB compiled into kernel. Kernel entry at 0x40200100... Kernel args: (null) ========================================================== Any suggestions? Thanks From owner-freebsd-arm@FreeBSD.ORG Tue Jun 18 21:38:44 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 90CDF7CF; Tue, 18 Jun 2013 21:38:44 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id 4396C1667; Tue, 18 Jun 2013 21:38:44 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5ILccuk095544; Tue, 18 Jun 2013 17:38:38 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5ILcc7G095543; Tue, 18 Jun 2013 21:38:38 GMT (envelope-from tinderbox@freebsd.org) Date: Tue, 18 Jun 2013 21:38:38 GMT Message-Id: <201306182138.r5ILcc7G095543@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 18 Jun 2013 21:38:44 -0000 TB --- 2013-06-18 18:40:18 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-18 18:40:18 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-18 18:40:18 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-18 18:40:18 - cleaning the object tree TB --- 2013-06-18 18:44:11 - /usr/local/bin/svn stat /src TB --- 2013-06-18 18:44:15 - At svn revision 251956 TB --- 2013-06-18 18:44:16 - building world TB --- 2013-06-18 18:44:16 - CROSS_BUILD_TESTING=YES TB --- 2013-06-18 18:44:16 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-18 18:44:16 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-18 18:44:16 - SRCCONF=/dev/null TB --- 2013-06-18 18:44:16 - TARGET=arm TB --- 2013-06-18 18:44:16 - TARGET_ARCH=arm TB --- 2013-06-18 18:44:16 - TZ=UTC TB --- 2013-06-18 18:44:16 - __MAKE_CONF=/dev/null TB --- 2013-06-18 18:44:16 - cd /src TB --- 2013-06-18 18:44:16 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Tue Jun 18 18:44:22 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools >>> stage 4.1: building includes >>> stage 4.2: building libraries >>> stage 4.3: make dependencies >>> stage 4.4: building everything [...] /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:183:34: note: expanded from macro 'APR_RING_PREV' #define APR_RING_PREV(ep, link) (ep)->link.prev ^ /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:177:34: note: expanded from macro 'APR_RING_NEXT' #define APR_RING_NEXT(ep, link) (ep)->link.next ^ fatal error: too many errors emitted, stopping now [-ferror-limit=] 1 warning and 20 errors generated. *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib/libapr *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib *** Error code 1 Stop. make: stopped in /src/usr.bin/svn *** Error code 1 Stop. make: stopped in /src/usr.bin *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-18 21:38:38 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-18 21:38:38 - ERROR: failed to build world TB --- 2013-06-18 21:38:38 - 8436.68 user 1439.36 system 10699.50 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 01:02:47 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 514C225B for ; Wed, 19 Jun 2013 01:02:47 +0000 (UTC) (envelope-from ganbold@gmail.com) Received: from mail-ie0-x22f.google.com (mail-ie0-x22f.google.com [IPv6:2607:f8b0:4001:c03::22f]) by mx1.freebsd.org (Postfix) with ESMTP id 2787B1F17 for ; Wed, 19 Jun 2013 01:02:47 +0000 (UTC) Received: by mail-ie0-f175.google.com with SMTP id a13so11779694iee.20 for ; Tue, 18 Jun 2013 18:02:46 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; bh=KRkDGHmmD46Y+QPqmzLQDYLJgJ/2EjfQiYFUW+SlYd0=; b=unpiRMCinzxTDXFiXPSGYkbeTtV8H4xkp/mXwqs/ftGm05kz+SsCdoWezCmClu4ukg AlJ8VkQV+Yvai0RQoGX6xjezfDvFxO9RhBQ+4CwFkikVoSHn+2ZvKuxXoQATsuPVkV8H 5D1IlOevmmlgoBAdSSqP8I8tanWaopkvJmgcsN7UeIZHi7cPBumDCxA27K4Bh4vWH9s1 d+g49n77WXdX+0pWgGfUykCn+mufwjzYh1V68UoQQqr8Wy8QzXPBJUqdL/mTI5RgRJj8 APFFiwuIGkJmPtcWrykPjSuLW9f8Xax79KWx9d9DqKGxposL/jU5/zU8Zt/mYG3reZ46 SgXg== MIME-Version: 1.0 X-Received: by 10.50.108.114 with SMTP id hj18mr9099373igb.87.1371603766855; Tue, 18 Jun 2013 18:02:46 -0700 (PDT) Received: by 10.64.235.239 with HTTP; Tue, 18 Jun 2013 18:02:46 -0700 (PDT) In-Reply-To: References: Date: Wed, 19 Jun 2013 09:02:46 +0800 Message-ID: Subject: Re: Booting problem on mele_a1000(Alwinner A10) From: Ganbold Tsagaankhuu To: Mariano Lescano Content-Type: text/plain; charset=ISO-8859-1 X-Content-Filtered-By: Mailman/MimeDel 2.1.14 Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 01:02:47 -0000 On Wed, Jun 19, 2013 at 5:03 AM, Mariano Lescano wrote: > Hi! > We are trying to run FreeBSD on mele_a1000(Allwiner a10). > At this moment we have running u-boot-sunxi-current with ethernet support > and compiled it with API and ELF support. > Also ubldr runs correctly, we can explore the file system and run all the > commands and kernel is loaded in memory. When we try to boot the kernel, > the boot process stops before printing the copyright output. This is the > console output we have: > > ========================================================== > ## Starting application at 0x48000054 ... > Consoles: U-Boot console > Compatible API signature found @5fe68100 > Number of U-Boot devices: 2 > > FreeBSD/armv6 U-Boot loader, Revision 1.2 > (root@mcvlab1, Fri Jun 7 16:34:55 ART 2013) > DRAM: 512MB > > Device: disk > - > /boot/kernel/kernel data=0x3862a4+0x17b004 syms=[0x4+0x6aed0+0x4+0x44d7e] > Hit [Enter] to boot immediately, or any other key for command prompt. > Booting [/boot/kernel/kernel]... > Using DTB compiled into kernel. > Kernel entry at 0x40200100... > Kernel args: (null) > ========================================================== > > Any suggestions? > People have problems booting r251709 or later on RPI, so I guess it would be the same on Mele. Can you try older revisions like r251703? Ganbold > Thanks > _______________________________________________ > freebsd-arm@freebsd.org mailing list > http://lists.freebsd.org/mailman/listinfo/freebsd-arm > To unsubscribe, send any mail to "freebsd-arm-unsubscribe@freebsd.org" > From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 05:27:38 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 4299059E; Wed, 19 Jun 2013 05:27:38 +0000 (UTC) (envelope-from tim@kientzle.com) Received: from monday.kientzle.com (99-115-135-74.uvs.sntcca.sbcglobal.net [99.115.135.74]) by mx1.freebsd.org (Postfix) with ESMTP id B14861A5A; Wed, 19 Jun 2013 05:27:37 +0000 (UTC) Received: (from root@localhost) by monday.kientzle.com (8.14.4/8.14.4) id r5J5RapC082783; Wed, 19 Jun 2013 05:27:36 GMT (envelope-from tim@kientzle.com) Received: from [192.168.2.123] (CiscoE3000 [192.168.1.65]) by kientzle.com with SMTP id p46stkkewj63qjtdr2p5uivdun; Wed, 19 Jun 2013 05:27:36 +0000 (UTC) (envelope-from tim@kientzle.com) Subject: Re: [head tinderbox] failure on arm/arm Mime-Version: 1.0 (Apple Message framework v1283) Content-Type: text/plain; charset=iso-8859-1 From: Tim Kientzle In-Reply-To: <201306182138.r5ILcc7G095543@freebsd-current.sentex.ca> Date: Tue, 18 Jun 2013 22:27:35 -0700 Content-Transfer-Encoding: quoted-printable Message-Id: References: <201306182138.r5ILcc7G095543@freebsd-current.sentex.ca> To: FreeBSD Tinderbox X-Mailer: Apple Mail (2.1283) Cc: arm@freebsd.org, current@freebsd.org, Peter Wemm X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 05:27:38 -0000 >>>> stage 4.2: building libraries >>>> stage 4.3: make dependencies >>>> stage 4.4: building everything > [...] > = /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:183= :34: note: expanded from macro 'APR_RING_PREV' > #define APR_RING_PREV(ep, link) (ep)->link.prev > ^ > = /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:177= :34: note: expanded from macro 'APR_RING_NEXT' > #define APR_RING_NEXT(ep, link) (ep)->link.next > ^ > fatal error: too many errors emitted, stopping now [-ferror-limit=3D] > 1 warning and 20 errors generated. > *** Error code 1 >=20 > Stop. > make: stopped in /src/usr.bin/svn/lib/libapr > *** Error code 1 This might be the OffsetOf bug for APR on ARM. We just got a fix pushed upstream for this a few days ago. I don't have time to look, but someone should take a peek at the following patch and see if it's needed: --- ./apr-1.4.7/include/apr_general.h.orig +++ ./apr-1.4.7/include/apr_general.h @@ -76,7 +76,7 @@ =B7*=B7@return=B7offset =B7*/ -#if=B7defined(CRAY)=B7||=B7(defined(__arm)=B7&&=B7!defined(LINUX)) = +#if=B7defined(CRAY)=B7||=B7(defined(__arm)=B7&&=B7!(defined(LINUX)=B7||=B7= defined(__FreeBSD__))) #ifdef=B7__STDC__ #define=B7APR_OFFSET(p_type,field)=B7_Offsetof(p_type,field) #else From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 05:39:35 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 2A5578CA for ; Wed, 19 Jun 2013 05:39:35 +0000 (UTC) (envelope-from f0andrey@gmail.com) Received: from mail-wg0-x22a.google.com (mail-wg0-x22a.google.com [IPv6:2a00:1450:400c:c00::22a]) by mx1.freebsd.org (Postfix) with ESMTP id B5E451AAB for ; Wed, 19 Jun 2013 05:39:34 +0000 (UTC) Received: by mail-wg0-f42.google.com with SMTP id z11so112872wgg.5 for ; Tue, 18 Jun 2013 22:39:33 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; bh=2qxFv0l8JxAK0lC/hu14tL/qgmZs61ilPlz2fg8bIN0=; b=U2NE5SkgCFP4HpLWC+XhU9iCL1gDXFHpwx2CQOrhECbM2iPUS24PDAv1APzZQ6HXbO Y0RIPfb0pCMzIDPlv/C3/LTdRrjhfBPSakPrZCRuoaMrTiiyJpcv6TLPnSlOkONyqjzc ymD8LGthtuLFrXHcQFNKXPUKh4UAT5XbL6H53e89Bw2GckoE3aR3QkPbShReP0ufo21E ZN/z9ahOxH7zUyf4Nz/xD5PsaOkS+3fT8a+5nh1MIA6jv5vAFdFD524nVxyLfvdqycx8 TNz6vlez0HFx8Ebmd7Vu6g1L4tFOo2GmEG2Xrk3iSoKdZbVlv9TGqg3riHBn4Hw+0R3b Y/Tg== MIME-Version: 1.0 X-Received: by 10.194.234.100 with SMTP id ud4mr815716wjc.44.1371620373783; Tue, 18 Jun 2013 22:39:33 -0700 (PDT) Received: by 10.194.240.132 with HTTP; Tue, 18 Jun 2013 22:39:33 -0700 (PDT) In-Reply-To: <51C0B3AA.3060304@yahoo.com> References: <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> <51C0B3AA.3060304@yahoo.com> Date: Wed, 19 Jun 2013 09:39:33 +0400 Message-ID: Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi From: Andrey Fesenko To: Sreekanth Rupavatharam Content-Type: text/plain; charset=UTF-8 Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 05:39:35 -0000 On Tue, Jun 18, 2013 at 11:23 PM, Sreekanth Rupavatharam wrote: > On 6/17/13 3:04 PM, Andrey Fesenko wrote: > > i'm rebuild devel/pcre > http://armv6.bsdnir.info.ipv4.sixxs.org/files/pcre_build.log > > are you build image on the system with blank /etc/make.conf? may be > you build clang version > # gcc -v > Using built-in specs. > Target: armv6-undermydesk-freebsd > Configured with: FreeBSD/armv6 system compiler > Thread model: posix > gcc version 4.2.1 20070831 patched [FreeBSD] > # g++ -v > Using built-in specs. > Target: armv6-undermydesk-freebsd > Configured with: FreeBSD/armv6 system compiler > Thread model: posix > gcc version 4.2.1 20070831 patched [FreeBSD] > > or you RPi have /etc/make.conf with clang > > I tried with clang and g++ with same error. Can you share your > /etc/make.conf? Sorry for not having replied, trying to collect the current and was offline /etc/make.conf empty on a system which builds the image, and RPi pi # cat /etc/make.conf WITH_PKGNG=yes # added by use.perl 2013-06-13 10:27:53 PERL_VERSION=5.14.4 Maybe you should try to build RPI-B kernel, just as I used to build script https://github.com/daveish/freebsd-arm-tools/ or my patchs https://bitbucket.org/f_andrey/freebsd-arm-tools/ From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 06:57:33 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id AEC56DDE for ; Wed, 19 Jun 2013 06:57:33 +0000 (UTC) (envelope-from a.buonanno@live.it) Received: from dub0-omc3-s6.dub0.hotmail.com (dub0-omc3-s6.dub0.hotmail.com [157.55.2.15]) by mx1.freebsd.org (Postfix) with ESMTP id 544011CEF for ; Wed, 19 Jun 2013 06:57:32 +0000 (UTC) Received: from DUB112-W70 ([157.55.2.8]) by dub0-omc3-s6.dub0.hotmail.com with Microsoft SMTPSVC(6.0.3790.4675); Tue, 18 Jun 2013 23:56:24 -0700 X-TMN: [oI/jXpwUCWjCcIdPu7DZUdjG9vSiiTwi] X-Originating-Email: [a.buonanno@live.it] Message-ID: From: Antonio Buonanno To: "freebsd-arm@freebsd.org" Subject: freebsd and ZigBee USB stick Date: Wed, 19 Jun 2013 08:56:25 +0200 Importance: Normal MIME-Version: 1.0 X-OriginalArrivalTime: 19 Jun 2013 06:56:24.0963 (UTC) FILETIME=[1D2E8D30:01CE6CBA] Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: quoted-printable X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 06:57:33 -0000 hi to all=2C i have this problem=2C i want use ZigBee USB Stick with freeb= sddo you think possible? do you have example=2C how to or other?best regads= Antonio = From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 07:14:45 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 97EDF4AF for ; Wed, 19 Jun 2013 07:14:45 +0000 (UTC) (envelope-from jmg@h2.funkthat.com) Received: from h2.funkthat.com (gate2.funkthat.com [208.87.223.18]) by mx1.freebsd.org (Postfix) with ESMTP id 7AC531D72 for ; Wed, 19 Jun 2013 07:14:45 +0000 (UTC) Received: from h2.funkthat.com (localhost [127.0.0.1]) by h2.funkthat.com (8.14.3/8.14.3) with ESMTP id r5J753K5094958 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Wed, 19 Jun 2013 00:05:03 -0700 (PDT) (envelope-from jmg@h2.funkthat.com) Received: (from jmg@localhost) by h2.funkthat.com (8.14.3/8.14.3/Submit) id r5J752WA094957; Wed, 19 Jun 2013 00:05:02 -0700 (PDT) (envelope-from jmg) Date: Wed, 19 Jun 2013 00:05:02 -0700 From: John-Mark Gurney To: Antonio Buonanno Subject: Re: freebsd and ZigBee USB stick Message-ID: <20130619070501.GG26412@funkthat.com> Mail-Followup-To: Antonio Buonanno , "freebsd-arm@freebsd.org" References: Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: User-Agent: Mutt/1.4.2.3i X-Operating-System: FreeBSD 7.2-RELEASE i386 X-PGP-Fingerprint: 54BA 873B 6515 3F10 9E88 9322 9CB1 8F74 6D3F A396 X-Files: The truth is out there X-URL: http://resnet.uoregon.edu/~gurney_j/ X-Resume: http://resnet.uoregon.edu/~gurney_j/resume.html X-to-the-FBI-CIA-and-NSA: HI! HOW YA DOIN? can i haz chizburger? X-Greylist: Sender IP whitelisted, not delayed by milter-greylist-4.2.2 (h2.funkthat.com [127.0.0.1]); Wed, 19 Jun 2013 00:05:03 -0700 (PDT) Cc: "freebsd-arm@freebsd.org" X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 07:14:45 -0000 Antonio Buonanno wrote this message on Wed, Jun 19, 2013 at 08:56 +0200: > hi to all, i have this problem, i want use ZigBee USB Stick with freebsddo you think possible? do you have example, how to or other?best regadsAntonio You need to be more specific since there are multiple different sticks... If it presents just a serial interface, like the XStick, it's likely easy to get functional.. The XStick looks like it uses the FTDI driver... I have one, but haven't tried to use it on my FreeBSD box... If it prevents another interface and there is linux software that uses libusb to interact w/ it, then it is probably doable w/ a bit of work... It all depends upon which one you have... -- John-Mark Gurney Voice: +1 415 225 5579 "All that I will do, has been done, All that I have, has not." From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 08:21:16 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 650B8A6; Wed, 19 Jun 2013 08:21:16 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id 18C861027; Wed, 19 Jun 2013 08:21:15 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5J8LFqE028577; Wed, 19 Jun 2013 04:21:15 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5J8LFUS028576; Wed, 19 Jun 2013 08:21:15 GMT (envelope-from tinderbox@freebsd.org) Date: Wed, 19 Jun 2013 08:21:15 GMT Message-Id: <201306190821.r5J8LFUS028576@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 08:21:16 -0000 TB --- 2013-06-19 05:20:18 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-19 05:20:18 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-19 05:20:18 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-19 05:20:18 - cleaning the object tree TB --- 2013-06-19 05:22:40 - /usr/local/bin/svn stat /src TB --- 2013-06-19 05:22:43 - At svn revision 251990 TB --- 2013-06-19 05:22:44 - building world TB --- 2013-06-19 05:22:44 - CROSS_BUILD_TESTING=YES TB --- 2013-06-19 05:22:44 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-19 05:22:44 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-19 05:22:44 - SRCCONF=/dev/null TB --- 2013-06-19 05:22:44 - TARGET=arm TB --- 2013-06-19 05:22:44 - TARGET_ARCH=arm TB --- 2013-06-19 05:22:44 - TZ=UTC TB --- 2013-06-19 05:22:44 - __MAKE_CONF=/dev/null TB --- 2013-06-19 05:22:44 - cd /src TB --- 2013-06-19 05:22:44 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Wed Jun 19 05:22:51 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools >>> stage 4.1: building includes >>> stage 4.2: building libraries >>> stage 4.3: make dependencies >>> stage 4.4: building everything [...] /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:183:34: note: expanded from macro 'APR_RING_PREV' #define APR_RING_PREV(ep, link) (ep)->link.prev ^ /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:177:34: note: expanded from macro 'APR_RING_NEXT' #define APR_RING_NEXT(ep, link) (ep)->link.next ^ fatal error: too many errors emitted, stopping now [-ferror-limit=] 1 warning and 20 errors generated. *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib/libapr *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib *** Error code 1 Stop. make: stopped in /src/usr.bin/svn *** Error code 1 Stop. make: stopped in /src/usr.bin *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-19 08:21:14 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-19 08:21:14 - ERROR: failed to build world TB --- 2013-06-19 08:21:14 - 8448.62 user 1462.31 system 10856.23 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 14:01:35 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 68B60D8A for ; Wed, 19 Jun 2013 14:01:35 +0000 (UTC) (envelope-from M.Reyelt@Brunel.de) Received: from mailer1.brunel.de (mailer1.brunel.de [57.66.180.133]) by mx1.freebsd.org (Postfix) with ESMTP id 2AB7E1365 for ; Wed, 19 Jun 2013 14:01:34 +0000 (UTC) Received: from mailer1.brunel.de (localhost [127.0.0.1]) by localhost (Postfix) with SMTP id DB746780188 for ; Wed, 19 Jun 2013 16:01:38 +0200 (CEST) Received: from mail-hv.brunel.de (mail-hv.brunellocal.de [192.168.1.234]) by mailer1.brunel.de (Postfix) with ESMTP id 97E4578010B for ; Wed, 19 Jun 2013 16:01:34 +0200 (CEST) Subject: Matthias Reyelt is out of office. From: M.Reyelt@Brunel.de To: freebsd-arm@freebsd.org Message-ID: Date: Wed, 19 Jun 2013 16:01:31 +0200 X-MIMETrack: Serialize by Router on HUB10149/Brunel/De(Release 7.0.4FP2|June 06, 2010) at 19.06.2013 04:01:34 PM MIME-Version: 1.0 Content-type: text/plain; charset=ISO-8859-1 Content-transfer-encoding: quoted-printable X-PMX-Version: 6.0.0.2142326, Antispam-Engine: 2.7.2.2107409, Antispam-Data: 2013.6.19.132434 X-Spam-Probability: Probability=8% X-Spam-Hits: HTML_00_01 0.05, HTML_00_10 0.05, BODYTEXTP_SIZE_3000_LESS 0, BODY_SIZE_1000_LESS 0, BODY_SIZE_100_199 0, BODY_SIZE_2000_LESS 0, BODY_SIZE_5000_LESS 0, BODY_SIZE_7000_LESS 0, BOUNCE_AUTORESP 0, BOUNCE_GENERIC 0, NO_REAL_NAME 0, NO_URI_FOUND 0, SMALL_BODY 0, __BOUNCE_AUTORESP_SUBJ 0, __CT 0, __CTE 0, __CT_TEXT_PLAIN 0, __HAS_FROM 0, __HAS_MSGID 0, __MIME_TEXT_ONLY 0, __MIME_VERSION 0, __SANE_MSGID 0, __TO_MALFORMED_2 0, __TO_NO_NAME 0 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 14:01:35 -0000 Ich werde ab Di, 06/18/2013 nicht im B=FCro sein. Ich kehre zur=FCck am= Do, 06/20/2013. I will respond to your message when I return on Friday 21. Regards Matthias= From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 18:15:34 2013 Return-Path: Delivered-To: freebsd-arm@FreeBSD.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 46D853FA; Wed, 19 Jun 2013 18:15:34 +0000 (UTC) (envelope-from zbb@semihalf.com) Received: from smtp.semihalf.com (smtp.semihalf.com [213.17.239.109]) by mx1.freebsd.org (Postfix) with ESMTP id B731B1682; Wed, 19 Jun 2013 18:15:33 +0000 (UTC) Received: from localhost (unknown [213.17.239.109]) by smtp.semihalf.com (Postfix) with ESMTP id 7001DC3CB7; Wed, 19 Jun 2013 20:15:26 +0200 (CEST) X-Virus-Scanned: by amavisd-new at semihalf.com Received: from smtp.semihalf.com ([213.17.239.109]) by localhost (smtp.semihalf.com [213.17.239.109]) (amavisd-new, port 10024) with ESMTP id dOmTgZ6v+Unl; Wed, 19 Jun 2013 20:15:25 +0200 (CEST) Received: from [10.0.2.117] (cardhu.semihalf.com [213.17.239.108]) by smtp.semihalf.com (Postfix) with ESMTPSA id E85DEC3AB7; Wed, 19 Jun 2013 20:15:24 +0200 (CEST) Message-ID: <51C1F53B.2080502@semihalf.com> Date: Wed, 19 Jun 2013 20:15:23 +0200 From: Zbyszek Bodek Organization: Semihalf User-Agent: Mozilla/5.0 (X11; Linux x86_64; rv:17.0) Gecko/20130510 Thunderbird/17.0.6 MIME-Version: 1.0 To: freebsd-current@freebsd.org Subject: Kernel build fails on ARM: Cannot fork: Cannot allocate memory X-Enigmail-Version: 1.5.1 Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit Cc: freebsd-arm@FreeBSD.org, jeff@FreeBSD.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 18:15:34 -0000 Hello, I've been trying to compile the kernel on my ARMv7 platform using the sources from the current FreeBSD HEAD. make buildkernel <.....> -j5 1/2 builds fails in the way described below: -------------------------------------------------------------------------- ing-include-dirs -fdiagnostics-show-option -nostdinc -I. -I/root/src/freebsd-arm-superpages/sys -I/root/src/freebsd-arm-superpages/sys/contrib/altq -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common -finline-limit=8000 --param inline-unit-growth=100 --param large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c Cannot fork: Cannot allocate memory *** [ffs_snapshot.o] Error code 2 1 error *** [buildkernel] Error code 2 1 error *** [buildkernel] Error code 2 1 error 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w -------------------------------------------------------------------------- The warning from std err is: -------------------------------------------------------------------------- vm_thread_new: kstack allocation failed vm_thread_new: kstack allocation failed -------------------------------------------------------------------------- I was trying to find out which commit is causing this (because I was previously working on some older revision) and using bisect I got to: -------------------------------------------------------------------------- Author: jeff Date: Tue Jun 18 04:50:20 2013 +0000 Refine UMA bucket allocation to reduce space consumption and improve performance. - Always free to the alloc bucket if there is space. This gives LIFO allocation order to improve hot-cache performance. This also allows for zones with a single bucket per-cpu rather than a pair if the entire working set fits in one bucket. - Enable per-cpu caches of buckets. To prevent recursive bucket allocation one bucket zone still has per-cpu caches disabled. - Pick the initial bucket size based on a table driven maximum size per-bucket rather than the number of items per-page. This gives more sane initial sizes. - Only grow the bucket size when we face contention on the zone lock, this causes bucket sizes to grow more slowly. - Adjust the number of items per-bucket to account for the header space. This packs the buckets more efficiently per-page while making them not quite powers of two. - Eliminate the per-zone free bucket list. Always return buckets back to the bucket zone. This ensures that as zones grow into larger bucket sizes they eventually discard the smaller sizes. It persists fewer buckets in the system. The locking is slightly trickier. - Only switch buckets in zalloc, not zfree, this eliminates pathological cases where we ping-pong between two buckets. - Ensure that the thread that fills a new bucket gets to allocate from it to give a better upper bound on allocation time. Sponsored by: EMC / Isilon Storage Division -------------------------------------------------------------------------- I checked this several times and this commits seems to be causing this. Does anyone observe similar behavior or have a solution? Best regards Zbyszek Bodek From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 18:22:43 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id BCC00876; Wed, 19 Jun 2013 18:22:43 +0000 (UTC) (envelope-from f0andrey@gmail.com) Received: from mail-we0-x22b.google.com (mail-we0-x22b.google.com [IPv6:2a00:1450:400c:c03::22b]) by mx1.freebsd.org (Postfix) with ESMTP id 2CE3C1711; Wed, 19 Jun 2013 18:22:43 +0000 (UTC) Received: by mail-we0-f171.google.com with SMTP id m46so4785077wev.30 for ; Wed, 19 Jun 2013 11:22:42 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; bh=RQ/shUQmXTrpOlorOymlScT7ShbHabxWCet3LvXFNyc=; b=1I+V3FFz3cvJVegwlqVY49P1OG85IG4WC11ttx3PVp3v2dAztECE6KQaedzFnTX4pn UcDup4BA1TWLTZNfOlX8ySDrhbUFQKFCCSCbC2t1mL/FD2RTf29UcnSdxq1nv2e0VWCN suBi3QUqYfd5IpNPt/FB630S47kuD2tLqvos/tiN1O0KIpdEs4tVLs6hFagDa9J6TLRl Y8Z7I9qHGQeATeM7by/kPAOSWiF49AB5K7JEMSJpNEAOV5C6Fy3qLEA37L1fdxKJgpOS OXIHHUvZIj4YiHHSNJc3c04qrN4RUQEsapR6mBdh3HmmZkwZffHI2E8Gy6h2e+xYlPdI 0qtw== MIME-Version: 1.0 X-Received: by 10.194.242.136 with SMTP id wq8mr3167767wjc.60.1371666162267; Wed, 19 Jun 2013 11:22:42 -0700 (PDT) Received: by 10.194.240.132 with HTTP; Wed, 19 Jun 2013 11:22:42 -0700 (PDT) In-Reply-To: <51C1F53B.2080502@semihalf.com> References: <51C1F53B.2080502@semihalf.com> Date: Wed, 19 Jun 2013 22:22:42 +0400 Message-ID: Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory From: Andrey Fesenko To: Zbyszek Bodek Content-Type: text/plain; charset=UTF-8 Cc: "freebsd-arm@freebsd.org" , freebsd-current X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 18:22:43 -0000 On Wed, Jun 19, 2013 at 10:15 PM, Zbyszek Bodek wrote: > Hello, > > I've been trying to compile the kernel on my ARMv7 platform using the > sources from the current FreeBSD HEAD. > > make buildkernel <.....> -j5 > > 1/2 builds fails in the way described below: > -------------------------------------------------------------------------- > ing-include-dirs -fdiagnostics-show-option -nostdinc -I. > -I/root/src/freebsd-arm-superpages/sys > -I/root/src/freebsd-arm-superpages/sys/contrib/altq > -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL > -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common > -finline-limit=8000 --param inline-unit-growth=100 --param > large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror > /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c > Cannot fork: Cannot allocate memory > *** [ffs_snapshot.o] Error code 2 > 1 error > *** [buildkernel] Error code 2 > 1 error > *** [buildkernel] Error code 2 > 1 error > 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w > -------------------------------------------------------------------------- > -j5 tricky :) I think it is necessary to build one may be in two streams, as well as make the swap From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 19:05:57 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 32CEEE9; Wed, 19 Jun 2013 19:05:57 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id DA9791973; Wed, 19 Jun 2013 19:05:56 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5JJ5tlo084127; Wed, 19 Jun 2013 15:05:55 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5JJ5t3J084120; Wed, 19 Jun 2013 19:05:55 GMT (envelope-from tinderbox@freebsd.org) Date: Wed, 19 Jun 2013 19:05:55 GMT Message-Id: <201306191905.r5JJ5t3J084120@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 19:05:57 -0000 TB --- 2013-06-19 16:10:16 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-19 16:10:16 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-19 16:10:16 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-19 16:10:16 - cleaning the object tree TB --- 2013-06-19 16:12:43 - /usr/local/bin/svn stat /src TB --- 2013-06-19 16:12:47 - At svn revision 251995 TB --- 2013-06-19 16:12:48 - building world TB --- 2013-06-19 16:12:48 - CROSS_BUILD_TESTING=YES TB --- 2013-06-19 16:12:48 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-19 16:12:48 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-19 16:12:48 - SRCCONF=/dev/null TB --- 2013-06-19 16:12:48 - TARGET=arm TB --- 2013-06-19 16:12:48 - TARGET_ARCH=arm TB --- 2013-06-19 16:12:48 - TZ=UTC TB --- 2013-06-19 16:12:48 - __MAKE_CONF=/dev/null TB --- 2013-06-19 16:12:48 - cd /src TB --- 2013-06-19 16:12:48 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Wed Jun 19 16:12:55 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools >>> stage 4.1: building includes >>> stage 4.2: building libraries >>> stage 4.3: make dependencies >>> stage 4.4: building everything [...] /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:183:34: note: expanded from macro 'APR_RING_PREV' #define APR_RING_PREV(ep, link) (ep)->link.prev ^ /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:177:34: note: expanded from macro 'APR_RING_NEXT' #define APR_RING_NEXT(ep, link) (ep)->link.next ^ fatal error: too many errors emitted, stopping now [-ferror-limit=] 1 warning and 20 errors generated. *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib/libapr *** Error code 1 Stop. make: stopped in /src/usr.bin/svn/lib *** Error code 1 Stop. make: stopped in /src/usr.bin/svn *** Error code 1 Stop. make: stopped in /src/usr.bin *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-19 19:05:55 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-19 19:05:55 - ERROR: failed to build world TB --- 2013-06-19 19:05:55 - 8433.58 user 1427.42 system 10538.94 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 20:01:28 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 08F9A4D9 for ; Wed, 19 Jun 2013 20:01:28 +0000 (UTC) (envelope-from mercanoles@gmail.com) Received: from mail-pa0-x232.google.com (mail-pa0-x232.google.com [IPv6:2607:f8b0:400e:c03::232]) by mx1.freebsd.org (Postfix) with ESMTP id D86C01C20 for ; Wed, 19 Jun 2013 20:01:27 +0000 (UTC) Received: by mail-pa0-f50.google.com with SMTP id fb1so5538237pad.37 for ; Wed, 19 Jun 2013 13:01:27 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :content-type; bh=F7G96u371oiRvpqnJyb6qP1LXaKGI18DVplFnSE7FGs=; b=fD4WLMr4cil3PZolWAXfck8swAjGDaZRWw+u9hBLCsHIMqfuV9sA/Z9luxU3K7EkLE 4AHz5CMkVGfpWVrDE1Y7H0SsJetE7Y38VZpEIJo8vHJtKaYfkXdFKu/w86LwrMiM8DNJ pdgJQmqfeF/A1eo/cVuJpNTCbABGGS2pQyN0IV6iETSpeUdqnN67E9OahkIOeRfmuW/F nQVTxeKaUY3zanTZNQaAXY/lbg42v7mD4CGUyVkKNBb3sV3YlKNefQQNSWe+/mEFfGuR 5hnYXiZlG5VHa1rJhffUwcYwYpjEmdkPXMWh6jVz35Bs4vsVqOi/dqNJi4pid1j8MHa1 ScTw== MIME-Version: 1.0 X-Received: by 10.66.218.39 with SMTP id pd7mr8149724pac.148.1371672087551; Wed, 19 Jun 2013 13:01:27 -0700 (PDT) Received: by 10.70.83.33 with HTTP; Wed, 19 Jun 2013 13:01:27 -0700 (PDT) In-Reply-To: References: Date: Wed, 19 Jun 2013 17:01:27 -0300 Message-ID: Subject: Fwd: Booting problem on mele_a1000(Alwinner A10) From: Mariano Lescano To: freebsd-arm@freebsd.org Content-Type: text/plain; charset=ISO-8859-1 X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 20:01:28 -0000 ---------- Forwarded message ---------- From: Mariano Lescano Date: 2013/6/19 Subject: Re: Booting problem on mele_a1000(Alwinner A10) To: Ganbold Tsagaankhuu Thanks for your answer. We are trying to install kernel-toolchains from r251703 without succes. This is the error: ======================================================= rm -f libncurses.so rm -f libncurses.a libncurses_p.a libncurses.so.8 rm -f .depend GPATH GRTAGS GSYMS GTAGS ===> lib/ncurses/form (cleandir) Unknown modifier 't' Error expanding embedded variable. *** Error code 2 Stop in /usr/src2/lib/ncurses. *** Error code 1 Stop in /usr/src2/lib. *** Error code 1 Stop in /usr/src2. *** Error code 1 Stop in /usr/src2. *** Error code 1 ====================================================== Any help is welcome... Thanks 2013/6/18 Ganbold Tsagaankhuu > > > > On Wed, Jun 19, 2013 at 5:03 AM, Mariano Lescano wrote: > >> Hi! >> We are trying to run FreeBSD on mele_a1000(Allwiner a10). >> At this moment we have running u-boot-sunxi-current with ethernet support >> and compiled it with API and ELF support. >> Also ubldr runs correctly, we can explore the file system and run all the >> commands and kernel is loaded in memory. When we try to boot the kernel, >> the boot process stops before printing the copyright output. This is the >> console output we have: >> >> ========================================================== >> ## Starting application at 0x48000054 ... >> Consoles: U-Boot console >> Compatible API signature found @5fe68100 >> Number of U-Boot devices: 2 >> >> FreeBSD/armv6 U-Boot loader, Revision 1.2 >> (root@mcvlab1, Fri Jun 7 16:34:55 ART 2013) >> DRAM: 512MB >> >> Device: disk >> - >> /boot/kernel/kernel data=0x3862a4+0x17b004 syms=[0x4+0x6aed0+0x4+0x44d7e] >> Hit [Enter] to boot immediately, or any other key for command prompt. >> Booting [/boot/kernel/kernel]... >> Using DTB compiled into kernel. >> Kernel entry at 0x40200100... >> Kernel args: (null) >> ========================================================== >> >> Any suggestions? >> > > > People have problems booting r251709 or later on RPI, so I guess it would > be the same on Mele. > Can you try older revisions like r251703? > > Ganbold > > > >> Thanks >> _______________________________________________ >> freebsd-arm@freebsd.org mailing list >> http://lists.freebsd.org/mailman/listinfo/freebsd-arm >> To unsubscribe, send any mail to "freebsd-arm-unsubscribe@freebsd.org" >> > > From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 21:09:58 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id E5D303EF for ; Wed, 19 Jun 2013 21:09:58 +0000 (UTC) (envelope-from ohauer@gmx.de) Received: from mout.gmx.net (mout.gmx.net [212.227.17.22]) by mx1.freebsd.org (Postfix) with ESMTP id 6A3B31F49 for ; Wed, 19 Jun 2013 21:09:58 +0000 (UTC) Received: from mailout-de.gmx.net ([10.1.76.35]) by mrigmx.server.lan (mrigmx002) with ESMTP (Nemesis) id 0M8ntS-1V1X7B2otY-00C8jo for ; Wed, 19 Jun 2013 23:09:57 +0200 Received: (qmail invoked by alias); 19 Jun 2013 21:09:57 -0000 Received: from p578be941.dip0.t-ipconnect.de (EHLO [192.168.0.100]) [87.139.233.65] by mail.gmx.net (mp035) with SMTP; 19 Jun 2013 23:09:57 +0200 X-Authenticated: #1956535 X-Provags-ID: V01U2FsdGVkX193G0AnCKR3O1i2LW3WkiI+bHpcUFVbt5rRzngt9s eClqGuvPcIRZCD Message-ID: <51C21E24.30306@gmx.de> Date: Wed, 19 Jun 2013 23:09:56 +0200 From: olli hauer User-Agent: Mozilla/5.0 (Windows NT 5.1; rv:17.0) Gecko/20130509 Thunderbird/17.0.6 MIME-Version: 1.0 To: Tim Kientzle Subject: Re: [head tinderbox] failure on arm/arm References: <201306182138.r5ILcc7G095543@freebsd-current.sentex.ca> In-Reply-To: X-Enigmail-Version: 1.5.1 Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 8bit X-Y-GMX-Trusted: 0 Cc: arm@freebsd.org, FreeBSD Tinderbox , Peter Wemm , current@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 21:09:59 -0000 On 2013-06-19 07:27, Tim Kientzle wrote:>>>>> stage 4.2: building libraries >>>>> stage 4.3: make dependencies >>>>> stage 4.4: building everything >> [...] >> /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:183:34: note: expanded from macro 'APR_RING_PREV' >> #define APR_RING_PREV(ep, link) (ep)->link.prev >> ^ >> /src/usr.bin/svn/lib/libapr/../../../../contrib/apr/include/apr_ring.h:177:34: note: expanded from macro 'APR_RING_NEXT' >> #define APR_RING_NEXT(ep, link) (ep)->link.next >> ^ >> fatal error: too many errors emitted, stopping now [-ferror-limit=] >> 1 warning and 20 errors generated. >> *** Error code 1 >> >> Stop. >> make: stopped in /src/usr.bin/svn/lib/libapr >> *** Error code 1 > > This might be the OffsetOf bug for APR on ARM. > We just got a fix pushed upstream for this a few > days ago. > > I don't have time to look, but someone should take > a peek at the following patch and see if it's > needed: > > --- ./apr-1.4.7/include/apr_general.h.orig > +++ ./apr-1.4.7/include/apr_general.h > @@ -76,7 +76,7 @@ > ·*·@return·offset > ·*/ > -#if·defined(CRAY)·||·(defined(__arm)·&&·!defined(LINUX)) > +#if·defined(CRAY)·||·(defined(__arm)·&&·!(defined(LINUX)·||·defined(__FreeBSD__))) > #ifdef·__STDC__ > #define·APR_OFFSET(p_type,field)·_Offsetof(p_type,field) > #else > Sorry for the late reply, There is a new apr version on the way which contains the fix already, I suspect it will be released during the next days (if no show stopper is found) The following patch updates apr from 1.4.6 to 1.4.8 http://people.freebsd.org/~ohauer/diffs/apr-1.4.8.1.4.1.diff Would you mind to test the new version on the arm platform and run $> make test (as non priv. user) I have tested on 8.4 and 9.1 no 10-cur system available, tests do not run on redports because of system restrictions (jail). -- olli From owner-freebsd-arm@FreeBSD.ORG Wed Jun 19 20:56:39 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id D06A2BD1 for ; Wed, 19 Jun 2013 20:56:39 +0000 (UTC) (envelope-from rskanth@yahoo.com) Received: from sam.nabble.com (sam.nabble.com [216.139.236.26]) by mx1.freebsd.org (Postfix) with ESMTP id B491B1E46 for ; Wed, 19 Jun 2013 20:56:39 +0000 (UTC) Received: from [192.168.236.26] (helo=sam.nabble.com) by sam.nabble.com with esmtp (Exim 4.72) (envelope-from ) id 1UpPQf-0004yE-0x for freebsd-arm@freebsd.org; Wed, 19 Jun 2013 13:56:33 -0700 Date: Wed, 19 Jun 2013 13:56:33 -0700 (PDT) From: rskanth To: freebsd-arm@freebsd.org Message-ID: <1371675392953-5821526.post@n5.nabble.com> In-Reply-To: References: <201306142359.r5ENxAes024505@oldred.freebsd.org> <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> <51C0B3AA.3060304@yahoo.com> Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Transfer-Encoding: 7bit X-Mailman-Approved-At: Wed, 19 Jun 2013 21:11:01 +0000 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 19 Jun 2013 20:56:39 -0000 All the roads are right now pointing to a clang issue on FreeBSD arm. The alignment issue originally noted by hiren is tracked in this PR. http://llvm.org/bugs/show_bug.cgi?id=15696. At this point I am keen on figuring out a) the Official way to cross-build ports on x86. I tried a few unofficial ones without success. I prefer this as it can significantly reduce build time b) completely disable clang in the native build on raspberry pi. I tried over-riding the /etc/make.conf with g++ for CXX and CPP, I get issues with the config. Any help is greatly appreciated. -- View this message in context: http://freebsd.1045724.n5.nabble.com/arm-179561-Compilation-issue-for-lighttpd-on-raspberry-pi-tp5820160p5821526.html Sent from the freebsd-arm mailing list archive at Nabble.com. From owner-freebsd-arm@FreeBSD.ORG Thu Jun 20 05:55:56 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id C21534BE for ; Thu, 20 Jun 2013 05:55:56 +0000 (UTC) (envelope-from villeinpuglia@libero.it) Received: from outrelay08.libero.it (outrelay08.libero.it [212.52.84.112]) by mx1.freebsd.org (Postfix) with ESMTP id 28E9A1B6D for ; Thu, 20 Jun 2013 05:55:55 +0000 (UTC) X-CTCH-Spam: Unknown X-CTCH-RefID: str=0001.0A0C0201.51C2996B.006C,ss=1,re=0.000,fgs=0 X-libjamoibt: 1823 Received: from serices.com (151.56.117.186) by outrelay08.libero.it (8.6.033) (authenticated as villeinpuglia@libero.it) id 51B90E1B014D1A99 for freebsd-arm@freebsd.org; Thu, 20 Jun 2013 07:55:55 +0200 MIME-Version: 1.0 From: "Informativa Immobiliare" To: freebsd-arm@freebsd.org Subject: Offerte Immobiliari Puglia X-Mailer: Smart_Send_2_0_138 Date: Thu, 20 Jun 2013 07:55:48 +0200 Message-ID: <33721915535443250119562@nxt-d98bdb07104> X-Antivirus: avast! (VPS 130619-1, 19/06/2013), Outbound message X-Antivirus-Status: Clean Content-Type: text/plain; charset="windows-1252" Content-Transfer-Encoding: quoted-printable X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list Reply-To: villeinpuglia@libero.it List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 20 Jun 2013 05:55:56 -0000 Buongiorno, pensando di farti cosa gradita ti informo che abbiamo alcune pr= oposte immobiliari in Puglia da proporti:=20 La prima proposta riguarda la vendita di una Villa a Santa Cesarea Terme ne= l Salento fronte mare. =20 La seconda proposta riguarda la vendita di una porzione di Villa di ampia m= etratura fronte mare nel Comune di Castro .=20 Per avere maggiori dettagli e visualizzare le foto delle proposte potete vi= sitare il sito web cliccando qui =20 Cordiali saluti Il contenuto di questa e-mail =E8 rivolto esclusivamente alle persone che u= tilizzano normalmente l'indirizzo di posta elettronica presso cui la presen= te =E8 stata spedita e pu=F2 contenere informazioni riservate o coperte da = segreto. Sono vietati la riproduzione, la comunicazione (inoltro) e la diff= usione di questa e-mail .Se avete ricevuto la presente e-mail per errore o = comunque non ne siete il destinatario vi invitiamo cortesemente a contattar= ci immediatamente per e-mail cencellando la mail originale Grazie=20 ---------------------------------------------------------------------------= ----- Good morning, thinking that you would appreciate this inform , we have to = propose you some properties in Puglia : The first proposal concerns the sale of a villa in Santa Cesarea Terme in S= alento in front of the sea.=20 The second proposal concerns the sale of a portion of a large size of a vil= la in front of the beach in the town of Castro.=20 For more details and for view some photos of the properties you can visit t= he website by clicking here Sincerely The contents of the e-mail is intended only to people who normally use the = email address from which this was sent and may contain confidential or priv= ileged. Reproduction, communication (forward) and dissemination of this e-m= ail. If you have received this e-mail by mistake or you are not the address= ee, please kindly contact us immediately by e-mail ridding the original ema= il Thanks From owner-freebsd-arm@FreeBSD.ORG Thu Jun 20 13:43:56 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id E8481D07 for ; Thu, 20 Jun 2013 13:43:56 +0000 (UTC) (envelope-from zbb@semihalf.com) Received: from mail-bk0-x234.google.com (mail-bk0-x234.google.com [IPv6:2a00:1450:4008:c01::234]) by mx1.freebsd.org (Postfix) with ESMTP id 77A321A26 for ; Thu, 20 Jun 2013 13:43:56 +0000 (UTC) Received: by mail-bk0-f52.google.com with SMTP id d7so2861409bkh.39 for ; Thu, 20 Jun 2013 06:43:55 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=message-id:date:from:organization:user-agent:mime-version:to:cc :subject:references:in-reply-to:content-type :content-transfer-encoding:x-gm-message-state; bh=iOLclm+MkryW2DydlBXQtcvucbPALMAVXQyT/ijFB4w=; b=FsvWC19hITRwvfQq913sGEZf1LLSimmnAqCzHWPXS/slVj11sQrHBABdF8SQARpNSf TkwTUPSvnwRiidMtdvUbeY0Bq0MZy7wCM+Em+dVgdH8hW38QObx0UN/34DE9ULoNgXwH ab8PqvafcofTL65z7WZojMS9K/w2YuIJo3zxlmPNY+QcInmYsFdE+YJEd/yapqgaYk52 keMaLYoM0uZbGpCYWEiZ4MW5p35bPu6lhNFVBVB8xuWo7FjGqoSi0/WcJeg3l2Qcb5pe jSi4Rtl7NpHYc5PZ3yCcNtY0ZNubPe3fX5ZISuFNufCqKKVh84smli1uDWzyWKnpDi70 0yig== X-Received: by 10.204.231.137 with SMTP id jq9mr1124019bkb.150.1371735835401; Thu, 20 Jun 2013 06:43:55 -0700 (PDT) Received: from [10.0.2.117] (cardhu.semihalf.com. [213.17.239.108]) by mx.google.com with ESMTPSA id eu16sm247855bkc.0.2013.06.20.06.43.53 for (version=TLSv1 cipher=ECDHE-RSA-RC4-SHA bits=128/128); Thu, 20 Jun 2013 06:43:54 -0700 (PDT) Message-ID: <51C30718.4030805@semihalf.com> Date: Thu, 20 Jun 2013 15:43:52 +0200 From: Zbyszek Bodek Organization: Semihalf User-Agent: Mozilla/5.0 (X11; Linux x86_64; rv:17.0) Gecko/20130510 Thunderbird/17.0.6 MIME-Version: 1.0 To: Andrey Fesenko Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory References: <51C1F53B.2080502@semihalf.com> In-Reply-To: Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 7bit X-Gm-Message-State: ALoCoQkpEhk+YhC7/C2+DyXESfkfY9SsOS1VforEBNwB6Yqy8auqMYKKbAnJ7b21A+hx0iFZNbjf Cc: "freebsd-arm@freebsd.org" , freebsd-current X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 20 Jun 2013 13:43:57 -0000 On 19.06.2013 20:22, Andrey Fesenko wrote: > On Wed, Jun 19, 2013 at 10:15 PM, Zbyszek Bodek wrote: >> Hello, >> >> I've been trying to compile the kernel on my ARMv7 platform using the >> sources from the current FreeBSD HEAD. >> >> make buildkernel <.....> -j5 >> >> 1/2 builds fails in the way described below: >> -------------------------------------------------------------------------- >> ing-include-dirs -fdiagnostics-show-option -nostdinc -I. >> -I/root/src/freebsd-arm-superpages/sys >> -I/root/src/freebsd-arm-superpages/sys/contrib/altq >> -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL >> -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common >> -finline-limit=8000 --param inline-unit-growth=100 --param >> large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror >> /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c >> Cannot fork: Cannot allocate memory >> *** [ffs_snapshot.o] Error code 2 >> 1 error >> *** [buildkernel] Error code 2 >> 1 error >> *** [buildkernel] Error code 2 >> 1 error >> 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w >> -------------------------------------------------------------------------- >> > > -j5 tricky :) I think it is necessary to build one may be in two > streams, as well as make the swap > Hello Andrey, I'm not sure whether you see my point. Just for the record, I've checked make <...> -j1 and with a swap file. The results are the same. Nevertheless, I have 2GB of main memory on my ARM target and this is more than sufficient to build the kernel without a necessity of swap, etc. What more, I never use more than ~300-400MB of memory during build even when the error occurs. What I'm saying is that, starting from the earlier mentioned commit I'm suffering from the Cannot fork: Cannot allocate memory + vm_thread_new: kstack allocation failed errors, while using exactly the same setup, etc. Best regards Zbyszek Bodek From owner-freebsd-arm@FreeBSD.ORG Thu Jun 20 14:06:59 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 9EC9D563 for ; Thu, 20 Jun 2013 14:06:59 +0000 (UTC) (envelope-from paul@gromit.dlib.vt.edu) Received: from lennier.cc.vt.edu (lennier.cc.vt.edu [198.82.162.213]) by mx1.freebsd.org (Postfix) with ESMTP id 5B6D31B7F for ; Thu, 20 Jun 2013 14:06:59 +0000 (UTC) Received: from zidane.cc.vt.edu (zidane.cc.vt.edu [198.82.163.227]) by lennier.cc.vt.edu (8.13.8/8.13.8) with ESMTP id r5KE1QuM021613; Thu, 20 Jun 2013 10:06:28 -0400 Received: from auth3.smtp.vt.edu (auth3.smtp.vt.edu [198.82.161.152]) by zidane.cc.vt.edu (MOS 4.3.3-GA) with ESMTP id YPO48802; Thu, 20 Jun 2013 10:06:28 -0400 X-Mirapoint-Received-SPF: 198.82.161.152 auth3.smtp.vt.edu 0 none X-Mirapoint-Received-SPF: 198.82.161.152 auth3.smtp.vt.edu 0 none Received: from pmather.tower.lib.vt.edu (pmather.tower.lib.vt.edu [128.173.51.28]) (authenticated bits=0) by auth3.smtp.vt.edu (8.13.8/8.13.8) with ESMTP id r5KE6S9b023267 (version=TLSv1/SSLv3 cipher=AES128-SHA bits=128 verify=NO); Thu, 20 Jun 2013 10:06:28 -0400 Content-Type: text/plain; charset=us-ascii Mime-Version: 1.0 (Mac OS X Mail 6.5 \(1508\)) Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi From: Paul Mather In-Reply-To: <1371675392953-5821526.post@n5.nabble.com> Date: Thu, 20 Jun 2013 10:06:28 -0400 Content-Transfer-Encoding: quoted-printable Message-Id: <20ECDE3B-8D7A-4DF4-A22C-5CC2552C7A66@gromit.dlib.vt.edu> References: <201306142359.r5ENxAes024505@oldred.freebsd.org> <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> <51C0B3AA.3060304@yahoo.com> <1371675392953-5821526.post@n5.nabble.com> To: rskanth X-Mailer: Apple Mail (2.1508) Cc: freebsd-arm@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 20 Jun 2013 14:06:59 -0000 On Jun 19, 2013, at 4:56 PM, rskanth wrote: > All the roads are right now pointing to a clang issue on FreeBSD arm. = The > alignment issue originally noted by hiren is tracked in this PR. > http://llvm.org/bugs/show_bug.cgi?id=3D15696. >=20 > At this point I am keen on figuring out > a) the Official way to cross-build ports on x86. I tried a few = unofficial > ones without success. I prefer this as it can significantly reduce = build > time I'd be very interested in hearing about successful port cross-building = strategies, too. I've used poudriere successfully to build x86 ports, = but it failed when trying to build for arm. It would be a big win for = me if I could add an arm pkgng repo to my poudriere build machine. > b) completely disable clang in the native build on raspberry pi. I = tried > over-riding the /etc/make.conf with g++ for CXX and CPP, I get issues = with > the config. I believe I've previously had success with this in /etc/src.conf: =3D=3D=3D=3D=3D CC=3Dgcc CXX=3Dg++ CPP=3Dgcpp =3D=3D=3D=3D=3D However, I haven't done a lot of native builds (maybe just one = successfully)---I have built using crochet on another machine most of = the time. Cheers, Paul.= From owner-freebsd-arm@FreeBSD.ORG Thu Jun 20 15:44:50 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 074B6F01 for ; Thu, 20 Jun 2013 15:44:50 +0000 (UTC) (envelope-from rskanth@yahoo.com) Received: from nm19-vm0.bullet.mail.bf1.yahoo.com (nm19-vm0.bullet.mail.bf1.yahoo.com [98.139.213.162]) by mx1.freebsd.org (Postfix) with ESMTP id AC66111A2 for ; Thu, 20 Jun 2013 15:44:48 +0000 (UTC) Received: from [98.139.212.152] by nm19.bullet.mail.bf1.yahoo.com with NNFMP; 20 Jun 2013 15:44:48 -0000 Received: from [98.139.213.14] by tm9.bullet.mail.bf1.yahoo.com with NNFMP; 20 Jun 2013 15:44:48 -0000 Received: from [127.0.0.1] by smtp114.mail.bf1.yahoo.com with NNFMP; 20 Jun 2013 15:44:48 -0000 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=yahoo.com; s=s1024; t=1371743088; bh=OpthjFOb69a1qS4A9/wyi1vDXyfPB/A6N8K84V2Q6VE=; h=X-Yahoo-Newman-Id:X-Yahoo-Newman-Property:X-YMail-OSG:X-Yahoo-SMTP:X-Rocket-Received:Message-ID:Date:From:User-Agent:MIME-Version:To:Subject:References:In-Reply-To:Content-Type; b=owKne4nLXlOAo1ESND499jFgr7sntXjhnST9AjaWYx+Jrkcj6pN7kae26yXPMKOxVkAKBmdHvHpcf6ovObdCqrVat3PyDpa6prJ4gvwAaRcPVQlLHKLQ1uKVwxemNkEfcJbd62HJF9CL8F5Puh2Aj0Jy3vRkNiPBJHxfyZDdq0c= X-Yahoo-Newman-Id: 72483.305.bm@smtp114.mail.bf1.yahoo.com X-Yahoo-Newman-Property: ymail-3 X-YMail-OSG: 7gmjbfwVM1n7lMAc8t3FVbNfQpcAJdM_mA4.hc2HOoCIxt1 g6Rgw76LW6GrCTCQiZ2y0l0HfkzovQuMcsyAK0npzVxebSMMZwfEwdwOGycm YQTbfqee3cRABWmzlxrPxDUE7OsLsGzNdYPQUu8zTN55s1RNVD2ffdOzURSQ MImkPbx3ZZGrlg.eYSDRK1hvGiMloTr72V4obtcr7sWZyD_UpaFlDoizKKrY NXnvPD4JyRICNwtUqYRLVOkoh4lRWwzjaR9VbaRiQa_T8elCk2JaqQ3jirb8 VVfzeC6PaQ9LozanDaDnuMOhhlB3CElk0aPSB0fJ_RIEpq9FHToHq7Rk519E unMadoorxsokiU57_.RfVyZUJctQvxzTqIoHhNZWWcZaY4qsrvuYitHzR93g R2N1k1aBn.55U5ZOPj1sLWnXDGAP3wAdRZVYztlxrx38XlxRBWcFty8iZ7yr 4KRpfpFb9uuZ7yh21KPyOvZo5onm9zEozQX4NFCQpsI6ZAY0y_uif0WeZ5A2 Y4iaZSB6WKZ9gMWxAl9spMVfU6CIdJMkeaQo08xQHXOvieFX0VAuqJs3Uedp Lk5bBb6X12.SD9R5TZpwlVDJwuc63mnQY.DHssFYWmj5MqxeU32ZBj_FQunZ dxBxkItAbLvRwy3bb6.7eiZ2ys8lf4RmmWA-- X-Yahoo-SMTP: 0vhBds2swBAUIWerZ77I22nIbgU- X-Rocket-Received: from sreekanth.voilavip.com (rskanth@24.130.110.113 with ) by smtp114.mail.bf1.yahoo.com with SMTP; 20 Jun 2013 08:44:48 -0700 PDT Message-ID: <51C3236E.6000507@yahoo.com> Date: Thu, 20 Jun 2013 08:44:46 -0700 From: Sreekanth Rupavatharam User-Agent: Mozilla/5.0 (Macintosh; Intel Mac OS X 10.8; rv:17.0) Gecko/20130509 Thunderbird/17.0.6 MIME-Version: 1.0 To: "freebsd-arm@freebsd.org" Subject: Re: arm/179561: Compilation issue for lighttpd on raspberry pi References: <201306142359.r5ENxAes024505@oldred.freebsd.org> <201306162210.r5GMA05N031413@freefall.freebsd.org> <51BF76F3.8020806@yahoo.com> <51C0B3AA.3060304@yahoo.com> <1371675392953-5821526.post@n5.nabble.com> <20ECDE3B-8D7A-4DF4-A22C-5CC2552C7A66@gromit.dlib.vt.edu> In-Reply-To: <20ECDE3B-8D7A-4DF4-A22C-5CC2552C7A66@gromit.dlib.vt.edu> Content-Type: text/plain; charset=ISO-8859-1; format=flowed Content-Transfer-Encoding: 7bit X-Content-Filtered-By: Mailman/MimeDel 2.1.14 X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 20 Jun 2013 15:44:50 -0000 Switching to g++ in make.conf caused it to fail with the following error. >/ ===> Building for pcre-8.32 />/ make all-am />/ CCLD pcretest />/ ./.libs/libpcre.so: undefined reference to `__clear_cache' />/ cc: error: linker command failed with exit code 1 (use -v to see invocation)/ Then I tried Rev r245446(Based on the discussion here http://lists.freebsd.org/pipermail/freebsd-arm/2013-January/004605.html and it seems to be not affected by the issue. Now I am able to build pcre natively on pi. I hope to try the same tree with cross-compilation today. -S From owner-freebsd-arm@FreeBSD.ORG Thu Jun 20 18:05:54 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 2331B52B for ; Thu, 20 Jun 2013 18:05:54 +0000 (UTC) (envelope-from jroberson@jroberson.net) Received: from mail-pd0-f174.google.com (mail-pd0-f174.google.com [209.85.192.174]) by mx1.freebsd.org (Postfix) with ESMTP id F360619B3 for ; Thu, 20 Jun 2013 18:05:53 +0000 (UTC) Received: by mail-pd0-f174.google.com with SMTP id 10so6489631pdc.33 for ; Thu, 20 Jun 2013 11:05:53 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=date:from:x-x-sender:to:cc:subject:in-reply-to:message-id :references:user-agent:mime-version:content-type:x-gm-message-state; bh=u1b/ZB3LKPj64lS/Jv3m1lZLv5F/0fk+SdRIL0juyb4=; b=c5bPDtjbAeBtb+9JhcaNSbx7/kaJdCmpeUBMFjpxL0h6xWAxTz/FqXELCoUJpEsYQn GEaqzabPznj+fYci1hUw2ZATGZ6gJejaw5VoBSHvUdwbSiKOhHUVouLvdv+9ynJeY7MJ PpWDYlUJvU3VW3bvTTjnOGrmvEcUulnz9o1DqxZcyAg/s+LRX/Qeq5iBkr5reJFVDdNq iw/0iw9PHwscON8PMFosGbm2/zXpPqyaAt2nrrTCj3lHPPGfhoBdiySFoxcT/4hWRK+Z xItG8qG0rcQg/opMDKhlCRm06XhACPHWk8NVXI+9gt3sWPDeK9blwSsYt0ZB1K52qoGJ 1K/g== X-Received: by 10.66.118.104 with SMTP id kl8mr12317044pab.182.1371751553188; Thu, 20 Jun 2013 11:05:53 -0700 (PDT) Received: from rrcs-66-91-135-210.west.biz.rr.com (rrcs-66-91-135-210.west.biz.rr.com. [66.91.135.210]) by mx.google.com with ESMTPSA id vb8sm1171354pbc.11.2013.06.20.11.05.51 for (version=TLSv1 cipher=RC4-SHA bits=128/128); Thu, 20 Jun 2013 11:05:52 -0700 (PDT) Date: Thu, 20 Jun 2013 07:58:34 -1000 (HST) From: Jeff Roberson X-X-Sender: jroberson@desktop To: Zbyszek Bodek Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory In-Reply-To: <51C1F53B.2080502@semihalf.com> Message-ID: References: <51C1F53B.2080502@semihalf.com> User-Agent: Alpine 2.00 (BSF 1167 2008-08-23) MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed X-Gm-Message-State: ALoCoQkDaBzAJpgJvUEktaLGeKpLsr3I/DwYwwgDcBhudEuOdS+PO2SL80u9Ac/gFT55cCsVmJXN Cc: freebsd-arm@FreeBSD.org, freebsd-current@freebsd.org, jeff@FreeBSD.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 20 Jun 2013 18:05:54 -0000 On Wed, 19 Jun 2013, Zbyszek Bodek wrote: > Hello, > > I've been trying to compile the kernel on my ARMv7 platform using the > sources from the current FreeBSD HEAD. > > make buildkernel <.....> -j5 > > 1/2 builds fails in the way described below: > -------------------------------------------------------------------------- > ing-include-dirs -fdiagnostics-show-option -nostdinc -I. > -I/root/src/freebsd-arm-superpages/sys > -I/root/src/freebsd-arm-superpages/sys/contrib/altq > -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL > -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common > -finline-limit=8000 --param inline-unit-growth=100 --param > large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror > /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c > Cannot fork: Cannot allocate memory > *** [ffs_snapshot.o] Error code 2 > 1 error > *** [buildkernel] Error code 2 > 1 error > *** [buildkernel] Error code 2 > 1 error > 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w > -------------------------------------------------------------------------- > > The warning from std err is: > -------------------------------------------------------------------------- > vm_thread_new: kstack allocation failed > vm_thread_new: kstack allocation failed > -------------------------------------------------------------------------- > > I was trying to find out which commit is causing this (because I was > previously working on some older revision) and using bisect I got to: > > -------------------------------------------------------------------------- > Author: jeff > Date: Tue Jun 18 04:50:20 2013 +0000 > > Refine UMA bucket allocation to reduce space consumption and improve > performance. > > - Always free to the alloc bucket if there is space. This gives LIFO > allocation order to improve hot-cache performance. This also allows > for zones with a single bucket per-cpu rather than a pair if the > entire > working set fits in one bucket. > - Enable per-cpu caches of buckets. To prevent recursive bucket > allocation one bucket zone still has per-cpu caches disabled. > - Pick the initial bucket size based on a table driven maximum size > per-bucket rather than the number of items per-page. This gives > more sane initial sizes. > - Only grow the bucket size when we face contention on the zone > lock, this > causes bucket sizes to grow more slowly. > - Adjust the number of items per-bucket to account for the header > space. > This packs the buckets more efficiently per-page while making them > not quite powers of two. > - Eliminate the per-zone free bucket list. Always return buckets back > to the bucket zone. This ensures that as zones grow into larger > bucket sizes they eventually discard the smaller sizes. It persists > fewer buckets in the system. The locking is slightly trickier. > - Only switch buckets in zalloc, not zfree, this eliminates > pathological > cases where we ping-pong between two buckets. > - Ensure that the thread that fills a new bucket gets to allocate from > it to give a better upper bound on allocation time. > > Sponsored by: EMC / Isilon Storage Division > -------------------------------------------------------------------------- > > I checked this several times and this commits seems to be causing this. Can you tell me how many cores and how much memory you have? And paste the output of vmstat -z when you see this error. You can try changing bucket_select() at line 339 in uma_core.c to read: static int bucket_select(int size) { return (MAX(PAGE_SIZE / size, 1)); } This will approximate the old bucket sizing behavior. Thanks, Jeff > > Does anyone observe similar behavior or have a solution? > > Best regards > Zbyszek Bodek > From owner-freebsd-arm@FreeBSD.ORG Fri Jun 21 00:03:29 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id C16BE26C for ; Fri, 21 Jun 2013 00:03:29 +0000 (UTC) (envelope-from jroberson@jroberson.net) Received: from mail-pa0-x22c.google.com (mail-pa0-x22c.google.com [IPv6:2607:f8b0:400e:c03::22c]) by mx1.freebsd.org (Postfix) with ESMTP id 9CC3B1DB4 for ; Fri, 21 Jun 2013 00:03:29 +0000 (UTC) Received: by mail-pa0-f44.google.com with SMTP id lj1so6951912pab.17 for ; Thu, 20 Jun 2013 17:03:29 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=date:from:x-x-sender:to:cc:subject:in-reply-to:message-id :references:user-agent:mime-version:content-type:x-gm-message-state; bh=uHRFq4tPH1oiN9uQQeMLwktKB0uusMHn6ky66SCDCi4=; b=Q0QBeNEnsodEMAELOCjc7GAWG5ecLcjPpcyJwuPl/QLUpFa2Ndv+QVsOAb8elAFUZc YJqR5rxaSSp64D+q3iqgRd01cpbfL73wVeaXKKXALQQlGnZftW60YVvkg+aBW75o/0Mn 6DyoonTMVpXdAmsUtet+cNiCxyN4poJYMmJfhK8e7mqXXEbZ42QPjHfKRtDpNLzGV1JX cY9pDJu/cRGUA+C3YRD82IGcpFN05tkrkxzDO4iEJwmto7yXwQ+Gvxn7wpTLytQr767F lc0P6AG0NB7xVcvvh2vRb+ZR+AUu5nO+Iy1Z7t9bCedri4AAdrytQ/ocngWXzuhEVbDx g2EQ== X-Received: by 10.68.228.201 with SMTP id sk9mr10077179pbc.4.1371773009310; Thu, 20 Jun 2013 17:03:29 -0700 (PDT) Received: from rrcs-66-91-135-210.west.biz.rr.com (rrcs-66-91-135-210.west.biz.rr.com. [66.91.135.210]) by mx.google.com with ESMTPSA id xe9sm2161347pbc.21.2013.06.20.17.03.27 for (version=TLSv1 cipher=RC4-SHA bits=128/128); Thu, 20 Jun 2013 17:03:28 -0700 (PDT) Date: Thu, 20 Jun 2013 13:56:10 -1000 (HST) From: Jeff Roberson X-X-Sender: jroberson@desktop To: Zbyszek Bodek Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory In-Reply-To: Message-ID: References: <51C1F53B.2080502@semihalf.com> User-Agent: Alpine 2.00 (BSF 1167 2008-08-23) MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed X-Gm-Message-State: ALoCoQkKdxYcYlEoRahqjMA24kpNYDuLI+Wx5IRfMZ9YNgOSYV9KJ4r7msc607brO0DfKEoCj6R7 Cc: freebsd-arm@FreeBSD.org, freebsd-current@freebsd.org, jeff@FreeBSD.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 21 Jun 2013 00:03:29 -0000 On Thu, 20 Jun 2013, Jeff Roberson wrote: > On Wed, 19 Jun 2013, Zbyszek Bodek wrote: > >> Hello, >> >> I've been trying to compile the kernel on my ARMv7 platform using the >> sources from the current FreeBSD HEAD. >> >> make buildkernel <.....> -j5 >> >> 1/2 builds fails in the way described below: >> -------------------------------------------------------------------------- >> ing-include-dirs -fdiagnostics-show-option -nostdinc -I. >> -I/root/src/freebsd-arm-superpages/sys >> -I/root/src/freebsd-arm-superpages/sys/contrib/altq >> -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL >> -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common >> -finline-limit=8000 --param inline-unit-growth=100 --param >> large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror >> /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c >> Cannot fork: Cannot allocate memory >> *** [ffs_snapshot.o] Error code 2 >> 1 error >> *** [buildkernel] Error code 2 >> 1 error >> *** [buildkernel] Error code 2 >> 1 error >> 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w >> -------------------------------------------------------------------------- >> >> The warning from std err is: >> -------------------------------------------------------------------------- >> vm_thread_new: kstack allocation failed >> vm_thread_new: kstack allocation failed >> -------------------------------------------------------------------------- >> >> I was trying to find out which commit is causing this (because I was >> previously working on some older revision) and using bisect I got to: >> >> -------------------------------------------------------------------------- >> Author: jeff >> Date: Tue Jun 18 04:50:20 2013 +0000 >> >> Refine UMA bucket allocation to reduce space consumption and improve >> performance. >> >> - Always free to the alloc bucket if there is space. This gives LIFO >> allocation order to improve hot-cache performance. This also allows >> for zones with a single bucket per-cpu rather than a pair if the >> entire >> working set fits in one bucket. >> - Enable per-cpu caches of buckets. To prevent recursive bucket >> allocation one bucket zone still has per-cpu caches disabled. >> - Pick the initial bucket size based on a table driven maximum size >> per-bucket rather than the number of items per-page. This gives >> more sane initial sizes. >> - Only grow the bucket size when we face contention on the zone >> lock, this >> causes bucket sizes to grow more slowly. >> - Adjust the number of items per-bucket to account for the header >> space. >> This packs the buckets more efficiently per-page while making them >> not quite powers of two. >> - Eliminate the per-zone free bucket list. Always return buckets back >> to the bucket zone. This ensures that as zones grow into larger >> bucket sizes they eventually discard the smaller sizes. It persists >> fewer buckets in the system. The locking is slightly trickier. >> - Only switch buckets in zalloc, not zfree, this eliminates >> pathological >> cases where we ping-pong between two buckets. >> - Ensure that the thread that fills a new bucket gets to allocate from >> it to give a better upper bound on allocation time. >> >> Sponsored by: EMC / Isilon Storage Division >> -------------------------------------------------------------------------- >> >> I checked this several times and this commits seems to be causing this. > > Can you tell me how many cores and how much memory you have? And paste the > output of vmstat -z when you see this error. > > You can try changing bucket_select() at line 339 in uma_core.c to read: > > static int > bucket_select(int size) > { > return (MAX(PAGE_SIZE / size, 1)); > } > > This will approximate the old bucket sizing behavior. Just to add some more information; On my machine with 16GB of ram the handful of recent UMA commits save about 20MB of kmem on boot. There are 30% fewer buckets allocated. And all of the malloc zones have similar amounts of cached space. Actually the page size malloc bucket is taking up much less space. I don't know if the problem is unique to arm but I have tested x86 limited to 512MB of ram without trouble. I will need the stats I mentioned before to understand what has happened. Jeff > > Thanks, > Jeff > >> >> Does anyone observe similar behavior or have a solution? >> >> Best regards >> Zbyszek Bodek >> > From owner-freebsd-arm@FreeBSD.ORG Fri Jun 21 00:56:32 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 518B67A3; Fri, 21 Jun 2013 00:56:32 +0000 (UTC) (envelope-from adrian.chadd@gmail.com) Received: from mail-qc0-x234.google.com (mail-qc0-x234.google.com [IPv6:2607:f8b0:400d:c01::234]) by mx1.freebsd.org (Postfix) with ESMTP id 07BB11F9F; Fri, 21 Jun 2013 00:56:31 +0000 (UTC) Received: by mail-qc0-f180.google.com with SMTP id a1so4229793qcx.11 for ; Thu, 20 Jun 2013 17:56:31 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=20120113; h=mime-version:sender:in-reply-to:references:date :x-google-sender-auth:message-id:subject:from:to:cc:content-type; bh=aVBLq/YeD8nefW0VC4KUyWCpESmMjkhGaGB54+Z9qmM=; b=sSiBlzelXHUlfOxY7nDdLLC2IUYsH74mIRxCLkFjIx7VnCLa2zDDfHCGRykgePWREV fXac2JI4MbEYMZ9oGfN790Y6lIMz3U72bIo6+/hF0T5fgWoLeJ2aqKM1RoTO3v+rnsV8 PoITabh/YVlCam1rILbEcyUzrAlXHy0vb1Nmvwc0Qw6psTcbwi2jGqqBJx3OiRHcNjkZ 6/V7nb9K7tTesctwJD5tVRA9LnS2PR8D6OYa1Q+Kp1DtU0JuC0yaoAgrMgrh8Z2fZnAJ S7bRhw940OYsXBouh/3HyOaRrMxr+jTqsJx3px9BmGa1B5+p2YukABB+RvODpVMWmci8 1n9g== MIME-Version: 1.0 X-Received: by 10.49.58.70 with SMTP id o6mr2543471qeq.1.1371776191560; Thu, 20 Jun 2013 17:56:31 -0700 (PDT) Sender: adrian.chadd@gmail.com Received: by 10.224.5.65 with HTTP; Thu, 20 Jun 2013 17:56:31 -0700 (PDT) In-Reply-To: References: <51C1F53B.2080502@semihalf.com> Date: Thu, 20 Jun 2013 17:56:31 -0700 X-Google-Sender-Auth: LBNSwJ9y55ug__MILUNEfwgUqVI Message-ID: Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory From: Adrian Chadd To: Jeff Roberson Content-Type: text/plain; charset=ISO-8859-1 Cc: freebsd-current@freebsd.org, freebsd-arm@freebsd.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 21 Jun 2013 00:56:32 -0000 On 20 June 2013 16:56, Jeff Roberson wrote: > Just to add some more information; On my machine with 16GB of ram the > handful of recent UMA commits save about 20MB of kmem on boot. There are > 30% fewer buckets allocated. And all of the malloc zones have similar > amounts of cached space. Actually the page size malloc bucket is taking up > much less space. > > I don't know if the problem is unique to arm but I have tested x86 limited > to 512MB of ram without trouble. I will need the stats I mentioned before > to understand what has happened. Have you tried lower than 512MB? Like, 128MB? I have a 128MB -HEAD VM on i386 and it's working fine but I haven't done much digging to see how _well_ its working. I'm about to try a 64MB and 96MB VM. I'd like to go all the way down to 32MB (obviously with a cut down kernel, as GENERIC is pretty damned big!) and ensure that i386 isn't behaving poorly. There are still plenty of ARM/MIPS embedded boards that ship with 32MB (and less) RAM. I'm going to try stable/9 on 128MB of RAM soon. I know that 9.1-REL i386 + 128MB RAM results in a crash. Hopefully this stuff is better on stable/9. Thanks, Adrian From owner-freebsd-arm@FreeBSD.ORG Fri Jun 21 01:26:47 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 649C9EF0 for ; Fri, 21 Jun 2013 01:26:47 +0000 (UTC) (envelope-from mcgovern@beta.com) Received: from spoon.beta.com (spoon.beta.com [199.165.180.2]) by mx1.freebsd.org (Postfix) with ESMTP id 15B8A110F for ; Fri, 21 Jun 2013 01:26:46 +0000 (UTC) Received: from [199.165.180.44] ([199.165.180.44]) by spoon.beta.com (8.14.5/8.14.5) with ESMTP id r5L1QXfb024437; Thu, 20 Jun 2013 21:26:33 -0400 (EDT) (envelope-from mcgovern@beta.com) Subject: Re: Two questions on -current... From: "Brian J. McGovern" To: Warner Losh In-Reply-To: <25ACCE84-5498-43EC-AD9D-D0CC17A8DB65@bsdimp.com> References: <1371521474.1391.9.camel@fbsd-laptop> <25ACCE84-5498-43EC-AD9D-D0CC17A8DB65@bsdimp.com> Content-Type: text/plain; charset="us-ascii" Organization: B.E.T.A. Date: Thu, 20 Jun 2013 21:26:31 -0400 Message-ID: <1371777991.1369.2.camel@fbsd-laptop> Mime-Version: 1.0 X-Mailer: Evolution 2.32.1 FreeBSD GNOME Team Port Content-Transfer-Encoding: 7bit X-Spam-Status: No, score=1.3 required=5.0 tests=RDNS_NONE autolearn=no version=3.3.2 X-Spam-Level: * X-Spam-Checker-Version: SpamAssassin 3.3.2 (2011-06-06) on spoon.beta.com Cc: freebsd-arm X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list Reply-To: mcgovern@beta.com List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 21 Jun 2013 01:26:47 -0000 On Mon, 2013-06-17 at 22:23 -0600, Warner Losh wrote: > On Jun 17, 2013, at 10:10 PM, Jason Birch wrote: > > 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: > > unknown target CPU 'armv5te', despite a find ... grep... on the code > > showing this option in both gcc and clang compilers and tools. Is this > > processor deprecated in current? Is there are a replacement? Did I miss > > a change in how to build the kernel (Currently using "make TARGET=arm > > TARGET_ARCH=arm KERNCONF=DB-88F6XXX buildkernel" in /usr/src)? > > > > You'll need TARGET_ARCH=armv6, I think. > > The Marvel Kirkwood are armv5te. > > I think the actual problem may be that no buildworld and/or kernel-toolchain was done first... > > Warner > > > Would this be a make XDEV=arm XDEV_ARCH=arm xdev? A buildworld and xdev had been done prior, but I have not specifically run a kernel-toolchain. The only thing I didn't try was to chroot in to the resulting directory in /usr. From owner-freebsd-arm@FreeBSD.ORG Fri Jun 21 02:10:57 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id D4B40704 for ; Fri, 21 Jun 2013 02:10:57 +0000 (UTC) (envelope-from imp@bsdimp.com) Received: from mail-ie0-x22a.google.com (mail-ie0-x22a.google.com [IPv6:2607:f8b0:4001:c03::22a]) by mx1.freebsd.org (Postfix) with ESMTP id A3EF012D1 for ; Fri, 21 Jun 2013 02:10:57 +0000 (UTC) Received: by mail-ie0-f170.google.com with SMTP id e11so18315510iej.15 for ; Thu, 20 Jun 2013 19:10:57 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=sender:subject:mime-version:content-type:from:in-reply-to:date:cc :content-transfer-encoding:message-id:references:to:x-mailer :x-gm-message-state; bh=gI9cfqeSJadOuPCnMwPpp55f/GiyRW+Mld4ybUB4LEE=; b=c5IZmph7vmi4T5/32+EBoMSWlGa7/d3XANZW7gSo+bMTulVSOqrz4bzWvNjw8opeKZ one/au88QR5rbFTM4JC3A38Q6OoM6lSLVU2Vk0dHZB3nVa0l3QN3j8zDMcdvavAcJIG6 XWLj/nICIxux8CcXJgKrscnkyLwLRfocKPPTeBN4/X+4MrtunIBdGK36Voy06z9xJZjM KJPcvQhUIbzjKc9gmZVQvsxaSPeDI30PhL4o+5iQnZ/1tqLpLmRZkZAImh9EZJrhSIaB Ccfh8jN3Xq+yuEnRynfKYftRow9tT99FAlLhVVdGCZZ4Io1qW7UwRlc+2zNQ/32+wXkg 5n9Q== X-Received: by 10.50.122.100 with SMTP id lr4mr1110919igb.18.1371780657342; Thu, 20 Jun 2013 19:10:57 -0700 (PDT) Received: from [10.0.0.53] (50-78-194-198-static.hfc.comcastbusiness.net. [50.78.194.198]) by mx.google.com with ESMTPSA id x10sm13853197igl.3.2013.06.20.19.10.55 for (version=TLSv1 cipher=ECDHE-RSA-RC4-SHA bits=128/128); Thu, 20 Jun 2013 19:10:56 -0700 (PDT) Sender: Warner Losh Subject: Re: Two questions on -current... Mime-Version: 1.0 (Apple Message framework v1085) Content-Type: text/plain; charset=us-ascii From: Warner Losh In-Reply-To: <1371777991.1369.2.camel@fbsd-laptop> Date: Thu, 20 Jun 2013 20:10:54 -0600 Content-Transfer-Encoding: quoted-printable Message-Id: <56BE33CD-D5E6-44F5-87E8-0B5116338E0A@bsdimp.com> References: <1371521474.1391.9.camel@fbsd-laptop> <25ACCE84-5498-43EC-AD9D-D0CC17A8DB65@bsdimp.com> <1371777991.1369.2.camel@fbsd-laptop> To: mcgovern@beta.com X-Mailer: Apple Mail (2.1085) X-Gm-Message-State: ALoCoQnHRn0EAKvedxrNTiFJFq/mDG7WV/i21otIxb/wZrEUW1XRl89Cjzq3zOsrQMOwewOO0ZVR Cc: freebsd-arm X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 21 Jun 2013 02:10:57 -0000 On Jun 20, 2013, at 7:26 PM, Brian J. McGovern wrote: > On Mon, 2013-06-17 at 22:23 -0600, Warner Losh wrote: >> On Jun 17, 2013, at 10:10 PM, Jason Birch wrote: >>> 2.) When trying to compile DB-88F6XXX, I'm getting an error "error: >>> unknown target CPU 'armv5te', despite a find ... grep... on the code >>> showing this option in both gcc and clang compilers and tools. Is = this >>> processor deprecated in current? Is there are a replacement? Did I = miss >>> a change in how to build the kernel (Currently using "make = TARGET=3Darm >>> TARGET_ARCH=3Darm KERNCONF=3DDB-88F6XXX buildkernel" in /usr/src)? >>>=20 >>> You'll need TARGET_ARCH=3Darmv6, I think.=20 >>=20 >> The Marvel Kirkwood are armv5te. >>=20 >> I think the actual problem may be that no buildworld and/or = kernel-toolchain was done first... >>=20 >> Warner >>=20 >>=20 >>=20 >=20 > Would this be a make XDEV=3Darm XDEV_ARCH=3Darm xdev? A buildworld and = xdev > had been done prior, but I have not specifically run a = kernel-toolchain. > The only thing I didn't try was to chroot in to the resulting = directory > in /usr. We don't have automatic support for using the XDEV-built compilers for = the kernel. External tool chains were added recently, but I haven't = taken it out for a spin yet... Warner From owner-freebsd-arm@FreeBSD.ORG Fri Jun 21 18:50:21 2013 Return-Path: Delivered-To: freebsd-arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [8.8.178.115]) by hub.freebsd.org (Postfix) with ESMTP id 3296978C for ; Fri, 21 Jun 2013 18:50:21 +0000 (UTC) (envelope-from zbb@semihalf.com) Received: from mail-bk0-x235.google.com (mail-bk0-x235.google.com [IPv6:2a00:1450:4008:c01::235]) by mx1.freebsd.org (Postfix) with ESMTP id A3FA21FB2 for ; Fri, 21 Jun 2013 18:50:20 +0000 (UTC) Received: by mail-bk0-f53.google.com with SMTP id e11so3450104bkh.26 for ; Fri, 21 Jun 2013 11:50:19 -0700 (PDT) X-Google-DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=20120113; h=message-id:date:from:organization:user-agent:mime-version:to:cc :subject:references:in-reply-to:content-type:x-gm-message-state; bh=yvFjdlRzTLubNvlq/m2Yapvhhaxs0P7N4Ni78If8QBo=; b=hu7cRlMtJCuSvMYY6EjMFRxJRaju3StPHDB5IvDMxcp4gaaEELMuZiAezYva1/xDQo F/OvOPN6BrO0xBz6OG9jLaLW8n2WBzbRtl/5YrrU9Y0aXK4TpQiI449LG/tkGVAZjrS+ 7of8DiwD7YsQZVCWDO5IOTSLmfnfaguXdWn36Np7uu2jys2GxWUUCKFwKAN537+SAzZa MQDHa5GM47aQO0+LKd7Salvt9NhhPx6vLPaXmRrdUeC5yIXZnTYta/job+RV4Y0hOGGX Ovcdi0TbhcN8zmmTTxYt2jyJJfoVtafM0j/UhdYEu+53yoZOP8yn9gSFkyPfiOQEpZ6J SjZw== X-Received: by 10.204.54.137 with SMTP id q9mr1935089bkg.80.1371840619574; Fri, 21 Jun 2013 11:50:19 -0700 (PDT) Received: from [10.0.2.117] (cardhu.semihalf.com. [213.17.239.108]) by mx.google.com with ESMTPSA id qw6sm2009033bkb.4.2013.06.21.11.50.17 for (version=TLSv1 cipher=ECDHE-RSA-RC4-SHA bits=128/128); Fri, 21 Jun 2013 11:50:18 -0700 (PDT) Message-ID: <51C4A067.7010203@semihalf.com> Date: Fri, 21 Jun 2013 20:50:15 +0200 From: Zbyszek Bodek Organization: Semihalf User-Agent: Mozilla/5.0 (X11; Linux x86_64; rv:17.0) Gecko/20130510 Thunderbird/17.0.6 MIME-Version: 1.0 To: Jeff Roberson Subject: Re: Kernel build fails on ARM: Cannot fork: Cannot allocate memory References: <51C1F53B.2080502@semihalf.com> In-Reply-To: Content-Type: multipart/mixed; boundary="------------040207010309000602070803" X-Gm-Message-State: ALoCoQnFURiTjDJDyUJQzUy7U/WoNANYhAAvW5NLK/bnhBjOsMrQqpJU0II4Sa+7xJ0DjafVA2FT X-Content-Filtered-By: Mailman/MimeDel 2.1.14 Cc: freebsd-arm@FreeBSD.org, freebsd-current@freebsd.org, jeff@FreeBSD.org X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 Precedence: list List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 21 Jun 2013 18:50:21 -0000 This is a multi-part message in MIME format. --------------040207010309000602070803 Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit On 21.06.2013 01:56, Jeff Roberson wrote: > On Thu, 20 Jun 2013, Jeff Roberson wrote: > >> On Wed, 19 Jun 2013, Zbyszek Bodek wrote: >> >>> Hello, >>> >>> I've been trying to compile the kernel on my ARMv7 platform using the >>> sources from the current FreeBSD HEAD. >>> >>> make buildkernel <.....> -j5 >>> >>> 1/2 builds fails in the way described below: >>> -------------------------------------------------------------------------- >>> >>> ing-include-dirs -fdiagnostics-show-option -nostdinc -I. >>> -I/root/src/freebsd-arm-superpages/sys >>> -I/root/src/freebsd-arm-superpages/sys/contrib/altq >>> -I/root/src/freebsd-arm-superpages/sys/contrib/libfdt -D_KERNEL >>> -DHAVE_KERNEL_OPTION_HEADERS -include opt_global.h -fno-common >>> -finline-limit=8000 --param inline-unit-growth=100 --param >>> large-function-growth=1000 -mno-thumb-interwork -ffreestanding -Werror >>> /root/src/freebsd-arm-superpages/sys/ufs/ffs/ffs_snapshot.c >>> Cannot fork: Cannot allocate memory >>> *** [ffs_snapshot.o] Error code 2 >>> 1 error >>> *** [buildkernel] Error code 2 >>> 1 error >>> *** [buildkernel] Error code 2 >>> 1 error >>> 5487.888u 481.569s 7:35.65 1310.0% 1443+167k 1741+5388io 221pf+0w >>> -------------------------------------------------------------------------- >>> >>> >>> The warning from std err is: >>> -------------------------------------------------------------------------- >>> >>> vm_thread_new: kstack allocation failed >>> vm_thread_new: kstack allocation failed >>> -------------------------------------------------------------------------- >>> >>> >>> I was trying to find out which commit is causing this (because I was >>> previously working on some older revision) and using bisect I got to: >>> >>> -------------------------------------------------------------------------- >>> >>> Author: jeff >>> Date: Tue Jun 18 04:50:20 2013 +0000 >>> >>> Refine UMA bucket allocation to reduce space consumption and improve >>> performance. >>> >>> - Always free to the alloc bucket if there is space. This gives >>> LIFO >>> allocation order to improve hot-cache performance. This also >>> allows >>> for zones with a single bucket per-cpu rather than a pair if the >>> entire >>> working set fits in one bucket. >>> - Enable per-cpu caches of buckets. To prevent recursive bucket >>> allocation one bucket zone still has per-cpu caches disabled. >>> - Pick the initial bucket size based on a table driven maximum size >>> per-bucket rather than the number of items per-page. This gives >>> more sane initial sizes. >>> - Only grow the bucket size when we face contention on the zone >>> lock, this >>> causes bucket sizes to grow more slowly. >>> - Adjust the number of items per-bucket to account for the header >>> space. >>> This packs the buckets more efficiently per-page while making them >>> not quite powers of two. >>> - Eliminate the per-zone free bucket list. Always return buckets >>> back >>> to the bucket zone. This ensures that as zones grow into larger >>> bucket sizes they eventually discard the smaller sizes. It >>> persists >>> fewer buckets in the system. The locking is slightly trickier. >>> - Only switch buckets in zalloc, not zfree, this eliminates >>> pathological >>> cases where we ping-pong between two buckets. >>> - Ensure that the thread that fills a new bucket gets to allocate >>> from >>> it to give a better upper bound on allocation time. >>> >>> Sponsored by: EMC / Isilon Storage Division >>> -------------------------------------------------------------------------- >>> >>> >>> I checked this several times and this commits seems to be causing this. >> >> Can you tell me how many cores and how much memory you have? And >> paste the output of vmstat -z when you see this error. >> >> You can try changing bucket_select() at line 339 in uma_core.c to read: >> >> static int >> bucket_select(int size) >> { >> return (MAX(PAGE_SIZE / size, 1)); >> } >> >> This will approximate the old bucket sizing behavior. > > Just to add some more information; On my machine with 16GB of ram the > handful of recent UMA commits save about 20MB of kmem on boot. There > are 30% fewer buckets allocated. And all of the malloc zones have > similar amounts of cached space. Actually the page size malloc bucket > is taking up much less space. > > I don't know if the problem is unique to arm but I have tested x86 > limited to 512MB of ram without trouble. I will need the stats I > mentioned before to understand what has happened. > Hello Jeff, Thank you for your interest in my problem. My system is a quad-core ARMv7 with 2048 MB of RAM on board. Please see attachment for the output from vmstat -z when the error occurs. Changing bucket_select() to static int bucket_select(int size) { return (MAX(PAGE_SIZE / size, 1)); } as you suggested helps for the problem. I've performed numerous attempts to build the kernel and none of them failed. Best regards Zbyszek Bodek --------------040207010309000602070803-- From owner-freebsd-arm@FreeBSD.ORG Sat Jun 22 00:46:36 2013 Return-Path: Delivered-To: arm@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by hub.freebsd.org (Postfix) with ESMTP id 31F2DA1F; Sat, 22 Jun 2013 00:46:36 +0000 (UTC) (envelope-from tinderbox@freebsd.org) Received: from freebsd-current.sentex.ca (freebsd-current.sentex.ca [64.7.128.98]) by mx1.freebsd.org (Postfix) with ESMTP id D09D41233; Sat, 22 Jun 2013 00:46:35 +0000 (UTC) Received: from freebsd-current.sentex.ca (localhost [127.0.0.1]) by freebsd-current.sentex.ca (8.14.5/8.14.5) with ESMTP id r5M0kT7Q047680; Fri, 21 Jun 2013 20:46:29 -0400 (EDT) (envelope-from tinderbox@freebsd.org) Received: (from tinderbox@localhost) by freebsd-current.sentex.ca (8.14.5/8.14.5/Submit) id r5M0kTth047679; Sat, 22 Jun 2013 00:46:29 GMT (envelope-from tinderbox@freebsd.org) Date: Sat, 22 Jun 2013 00:46:29 GMT Message-Id: <201306220046.r5M0kTth047679@freebsd-current.sentex.ca> X-Authentication-Warning: freebsd-current.sentex.ca: tinderbox set sender to FreeBSD Tinderbox using -f Sender: FreeBSD Tinderbox From: FreeBSD Tinderbox To: FreeBSD Tinderbox , , Subject: [head tinderbox] failure on arm/arm Precedence: bulk X-BeenThere: freebsd-arm@freebsd.org X-Mailman-Version: 2.1.14 List-Id: Porting FreeBSD to the StrongARM Processor List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 22 Jun 2013 00:46:36 -0000 TB --- 2013-06-22 00:20:18 - tinderbox 2.10 running on freebsd-current.sentex.ca TB --- 2013-06-22 00:20:18 - FreeBSD freebsd-current.sentex.ca 8.3-PRERELEASE FreeBSD 8.3-PRERELEASE #0: Mon Mar 26 13:54:12 EDT 2012 des@freebsd-current.sentex.ca:/usr/obj/usr/src/sys/GENERIC amd64 TB --- 2013-06-22 00:20:18 - starting HEAD tinderbox run for arm/arm TB --- 2013-06-22 00:20:18 - cleaning the object tree TB --- 2013-06-22 00:20:18 - /usr/local/bin/svn stat /src TB --- 2013-06-22 00:20:23 - At svn revision 252079 TB --- 2013-06-22 00:20:24 - building world TB --- 2013-06-22 00:20:24 - CROSS_BUILD_TESTING=YES TB --- 2013-06-22 00:20:24 - MAKEOBJDIRPREFIX=/obj TB --- 2013-06-22 00:20:24 - PATH=/usr/bin:/usr/sbin:/bin:/sbin TB --- 2013-06-22 00:20:24 - SRCCONF=/dev/null TB --- 2013-06-22 00:20:24 - TARGET=arm TB --- 2013-06-22 00:20:24 - TARGET_ARCH=arm TB --- 2013-06-22 00:20:24 - TZ=UTC TB --- 2013-06-22 00:20:24 - __MAKE_CONF=/dev/null TB --- 2013-06-22 00:20:24 - cd /src TB --- 2013-06-22 00:20:24 - /usr/bin/make -B buildworld >>> Building an up-to-date make(1) >>> World build started on Sat Jun 22 00:20:30 UTC 2013 >>> Rebuilding the temporary build tree >>> stage 1.1: legacy release compatibility shims >>> stage 1.2: bootstrap tools >>> stage 2.1: cleaning up the object tree >>> stage 2.2: rebuilding the object tree >>> stage 2.3: build tools >>> stage 3: cross tools [...] c++ -O2 -pipe -I/src/lib/clang/libclangparse/../../../contrib/llvm/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse -I. -I/src/lib/clang/libclangparse/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse/ParseOpenMP.cpp -o ParseOpenMP.o c++ -O2 -pipe -I/src/lib/clang/libclangparse/../../../contrib/llvm/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse -I. -I/src/lib/clang/libclangparse/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse/ParsePragma.cpp -o ParsePragma.o c++ -O2 -pipe -I/src/lib/clang/libclangparse/../../../contrib/llvm/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/include -I/src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse -I. -I/src/lib/clang/libclangparse/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse/ParseStmt.cpp -o ParseStmt.o /src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse/ParseStmt.cpp: In member function 'clang::StmtResult clang::Parser::ParseDoStatement()': /src/lib/clang/libclangparse/../../../contrib/llvm/tools/clang/lib/Parse/ParseStmt.cpp:1250: internal compiler error: Segmentation fault: 11 Please submit a full bug report, with preprocessed source if appropriate. See for instructions. *** Error code 1 Stop. make: stopped in /src/lib/clang/libclangparse *** Error code 1 Stop. make: stopped in /src/lib/clang ===> lib/clang/include (install) sh /src/tools/install.sh -C -o root -g wheel -m 444 /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/__wmmintrin_aes.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/__wmmintrin_pclmul.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/altivec.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/ammintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/avx2intrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/avxintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/bmi2intrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/bmiintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/cpuid.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/emmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/f16cintrin.h /src/lib/clang/include/../../../c! ontrib/llvm/tools/clang/lib/Headers/fma4intrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/fmaintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/immintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/lzcntintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/mm3dnow.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/mm_malloc.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/mmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/module.map /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/nmmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/pmmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/popcntintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/prfchwintrin.h /src/lib/clang/include/../../../contrib/llvm! /tools/clang/lib/Headers/rdseedintrin.h /src/lib/clang/include! /../../../contrib/llvm/tools/clang/lib/Headers/rtmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/smmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/tmmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/wmmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/x86intrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/xmmintrin.h /src/lib/clang/include/../../../contrib/llvm/tools/clang/lib/Headers/xopintrin.h /obj/arm.arm/src/tmp/usr/include/clang/3.3 ===> usr.bin/clang (obj,depend,all,install) ===> usr.bin/clang/clang (obj) /obj/arm.arm/src/tmp/src/usr.bin/clang/clang created for /src/usr.bin/clang/clang ===> usr.bin/clang/clang-tblgen (obj) ===> usr.bin/clang/tblgen (obj) ===> usr.bin/clang/clang (depend) clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Driver -gen-opt-parser-defs -o CC1AsOptions.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Driver/CC1AsOptions.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic -gen-clang-diags-defs -clang-component=Common -o DiagnosticCommonKinds.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic/Diagnostic.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic -gen-clang-diags-defs -clang-component=Driver -o DiagnosticDriverKinds.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic/Diagnostic.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic -gen-clang-diags-defs -clang-component=Frontend -o DiagnosticFrontendKinds.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic/Diagnostic.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic -gen-clang-diags-defs -clang-component=Lex -o DiagnosticLexKinds.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic/Diagnostic.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic -gen-clang-diags-defs -clang-component=Sema -o DiagnosticSemaKinds.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Basic/Diagnostic.td clang-tblgen -I /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Driver -gen-opt-parser-defs -o Options.inc.h /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include/clang/Driver/Options.td rm -f .depend mkdep -f .depend -a -I/src/usr.bin/clang/clang/../../../contrib/llvm/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver -I. -I/src/usr.bin/clang/clang/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/cc1_main.cpp /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/cc1as_main.cpp /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/driver.cpp echo clang: /usr/lib/libc.a CC1AsOptions.inc.h DiagnosticCommonKinds.inc.h DiagnosticDriverKinds.inc.h DiagnosticFrontendKinds.inc.h DiagnosticLexKinds.inc.h DiagnosticSemaKinds.inc.h Options.inc.h /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangfrontendtool/libclangfrontendtool.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangfrontend/libclangfrontend.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangdriver/libclangdriver.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangserialization/libclangserialization.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangcodegen/libclangcodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangparse/libclangparse.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangsema/libclangsema.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclanganalysis/libclanganal! ysis.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangedit/libclangedit.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangast/libclangast.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangbasic/libclangbasic.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclanglex/libclanglex.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmlinker/libllvmlinker.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmirreader/libllvmirreader.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipo/libllvmipo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmvectorize/libllvmvectorize.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstrumentation/libllvminstrumentation.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitwriter/libllvmbitwriter.a /obj/arm.arm/src/tmp/sr! c/usr.bin/clang/clang/../../../lib/clang/libllvmbitreader/libl! lvmbitreader.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmparser/libllvmasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdisassembler/libllvmarmdisassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmcodegen/libllvmarmcodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmasmparser/libllvmarmasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdesc/libllvmarmdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminfo/libllvmarminfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminstprinter/libllvmarminstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdisassembler/libllvmmipsdisassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipscodegen/libllvmmipscodegen.a /obj/arm.arm/src/tmp/src/usr.bin/! clang/clang/../../../lib/clang/libllvmmipsasmparser/libllvmmipsasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdesc/libllvmmipsdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinfo/libllvmmipsinfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinstprinter/libllvmmipsinstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpccodegen/libllvmpowerpccodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcdesc/libllvmpowerpcdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinfo/libllvmpowerpcinfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinstprinter/libllvmpowerpcinstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86disassembler/libllvmx86disassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib! /clang/libllvmx86asmparser/libllvmx86asmparser.a /obj/arm.arm/src/tmp/s! rc/usr.bin/clang/clang/../../../lib/clang/libllvmx86codegen/libllvmx86codegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmselectiondag/libllvmselectiondag.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmprinter/libllvmasmprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmcparser/libllvmmcparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcodegen/libllvmcodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobjcarcopts/libllvmobjcarcopts.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmscalaropts/libllvmscalaropts.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstcombine/libllvminstcombine.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtransformutils/libllvmtransformutils.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipa/libllvmipa.! a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmanalysis/libllvmanalysis.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86desc/libllvmx86desc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86info/libllvmx86info.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtarget/libllvmtarget.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86instprinter/libllvmx86instprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmc/libllvmmc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobject/libllvmobject.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86utils/libllvmx86utils.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcore/libllvmcore.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmsupport/libllvmsupport.a /obj/arm.arm/src/tmp/legacy/! usr/lib/libegacy.a >> .depend echo clang: /usr/lib/libstdc++.a >> .depend ===> usr.bin/clang/clang-tblgen (depend) ===> usr.bin/clang/tblgen (depend) ===> usr.bin/clang/clang (all) c++ -O2 -pipe -I/src/usr.bin/clang/clang/../../../contrib/llvm/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver -I. -I/src/usr.bin/clang/clang/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/cc1_main.cpp c++ -O2 -pipe -I/src/usr.bin/clang/clang/../../../contrib/llvm/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver -I. -I/src/usr.bin/clang/clang/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/cc1as_main.cpp c++ -O2 -pipe -I/src/usr.bin/clang/clang/../../../contrib/llvm/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver -I. -I/src/usr.bin/clang/clang/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -c /src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver/driver.cpp make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangserialization/libclangserialization.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangparse/libclangparse.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangsema/libclangsema.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmlinker/libllvmlinker.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmirreader/libllvmirreader.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipo/libllvmipo.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmvectorize/libllvmvectorize.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstrumentation/libllvminstrumentation.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitwriter/libllvmbitwriter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitreader/libllvmbitreader.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmparser/libllvmasmparser.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdisassembler/libllvmarmdisassembler.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmcodegen/libllvmarmcodegen.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmasmparser/libllvmarmasmparser.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdesc/libllvmarmdesc.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminfo/libllvmarminfo.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminstprinter/libllvmarminstprinter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdisassembler/libllvmmipsdisassembler.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipscodegen/libllvmmipscodegen.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsasmparser/libllvmmipsasmparser.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdesc/libllvmmipsdesc.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinfo/libllvmmipsinfo.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinstprinter/libllvmmipsinstprinter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpccodegen/libllvmpowerpccodegen.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcdesc/libllvmpowerpcdesc.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinfo/libllvmpowerpcinfo.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinstprinter/libllvmpowerpcinstprinter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86disassembler/libllvmx86disassembler.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86asmparser/libllvmx86asmparser.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86codegen/libllvmx86codegen.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmselectiondag/libllvmselectiondag.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmprinter/libllvmasmprinter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmcparser/libllvmmcparser.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcodegen/libllvmcodegen.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobjcarcopts/libllvmobjcarcopts.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmscalaropts/libllvmscalaropts.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstcombine/libllvminstcombine.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtransformutils/libllvmtransformutils.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipa/libllvmipa.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmanalysis/libllvmanalysis.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86desc/libllvmx86desc.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86info/libllvmx86info.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtarget/libllvmtarget.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86instprinter/libllvmx86instprinter.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmc/libllvmmc.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobject/libllvmobject.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86utils/libllvmx86utils.a make: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/.depend, 978: ignoring stale .depend for /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcore/libllvmcore.a c++ -O2 -pipe -I/src/usr.bin/clang/clang/../../../contrib/llvm/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/include -I/src/usr.bin/clang/clang/../../../contrib/llvm/tools/clang/tools/driver -I. -I/src/usr.bin/clang/clang/../../../contrib/llvm/../../lib/clang/include -DLLVM_ON_UNIX -DLLVM_ON_FREEBSD -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -fno-strict-aliasing -DLLVM_DEFAULT_TARGET_TRIPLE=\"arm-unknown-freebsd10.0\" -DLLVM_HOST_TRIPLE=\"x86_64-unknown-freebsd10.0\" -DDEFAULT_SYSROOT=\"/obj/arm.arm/src/tmp\" -I/obj/arm.arm/src/tmp/legacy/usr/include -fno-exceptions -fno-rtti -static -L/obj/arm.arm/src/tmp/legacy/usr/lib -o clang cc1_main.o cc1as_main.o driver.o /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangfrontendtool/libclangfrontendtool.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangfrontend/libclangfrontend.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangdriver/lib! clangdriver.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangserialization/libclangserialization.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangcodegen/libclangcodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangparse/libclangparse.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangsema/libclangsema.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclanganalysis/libclanganalysis.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangedit/libclangedit.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangast/libclangast.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangbasic/libclangbasic.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclanglex/libclanglex.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmlinker/libllvmlinker.a /obj/arm.arm/src/tmp! /src/usr.bin/clang/clang/../../../lib/clang/libllvmirreader/li! bllvmirreader.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipo/libllvmipo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmvectorize/libllvmvectorize.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstrumentation/libllvminstrumentation.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitwriter/libllvmbitwriter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitreader/libllvmbitreader.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmparser/libllvmasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdisassembler/libllvmarmdisassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmcodegen/libllvmarmcodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmasmparser/libllvmarmasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../.! ./lib/clang/libllvmarmdesc/libllvmarmdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminfo/libllvmarminfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminstprinter/libllvmarminstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdisassembler/libllvmmipsdisassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipscodegen/libllvmmipscodegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsasmparser/libllvmmipsasmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdesc/libllvmmipsdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinfo/libllvmmipsinfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinstprinter/libllvmmipsinstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpccodegen/libllvmpowerpccode! gen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/l! ibllvmpowerpcdesc/libllvmpowerpcdesc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinfo/libllvmpowerpcinfo.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinstprinter/libllvmpowerpcinstprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86disassembler/libllvmx86disassembler.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86asmparser/libllvmx86asmparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86codegen/libllvmx86codegen.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmselectiondag/libllvmselectiondag.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmprinter/libllvmasmprinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmcparser/libllvmmcparser.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcodegen/libllvmcodegen.a /obj/! arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobjcarcopts/libllvmobjcarcopts.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmscalaropts/libllvmscalaropts.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstcombine/libllvminstcombine.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtransformutils/libllvmtransformutils.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipa/libllvmipa.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmanalysis/libllvmanalysis.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86desc/libllvmx86desc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86info/libllvmx86info.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtarget/libllvmtarget.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86instprinter/libllvmx86instp! rinter.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clan! g/libllvmmc/libllvmmc.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobject/libllvmobject.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86utils/libllvmx86utils.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcore/libllvmcore.a /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmsupport/libllvmsupport.a -legacy c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangserialization/libclangserialization.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangparse/libclangparse.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libclangsema/libclangsema.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmlinker/libllvmlinker.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmirreader/libllvmirreader.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipo/libllvmipo.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmvectorize/libllvmvectorize.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstrumentation/libllvminstrumentation.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitwriter/libllvmbitwriter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmbitreader/libllvmbitreader.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmparser/libllvmasmparser.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdisassembler/libllvmarmdisassembler.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmcodegen/libllvmarmcodegen.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmasmparser/libllvmarmasmparser.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarmdesc/libllvmarmdesc.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminfo/libllvmarminfo.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmarminstprinter/libllvmarminstprinter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdisassembler/libllvmmipsdisassembler.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipscodegen/libllvmmipscodegen.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsasmparser/libllvmmipsasmparser.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsdesc/libllvmmipsdesc.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinfo/libllvmmipsinfo.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmipsinstprinter/libllvmmipsinstprinter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpccodegen/libllvmpowerpccodegen.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcdesc/libllvmpowerpcdesc.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinfo/libllvmpowerpcinfo.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmpowerpcinstprinter/libllvmpowerpcinstprinter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86disassembler/libllvmx86disassembler.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86asmparser/libllvmx86asmparser.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86codegen/libllvmx86codegen.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmselectiondag/libllvmselectiondag.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmasmprinter/libllvmasmprinter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmcparser/libllvmmcparser.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcodegen/libllvmcodegen.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobjcarcopts/libllvmobjcarcopts.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmscalaropts/libllvmscalaropts.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvminstcombine/libllvminstcombine.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtransformutils/libllvmtransformutils.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmipa/libllvmipa.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmanalysis/libllvmanalysis.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86desc/libllvmx86desc.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86info/libllvmx86info.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmtarget/libllvmtarget.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86instprinter/libllvmx86instprinter.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmmc/libllvmmc.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmobject/libllvmobject.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmx86utils/libllvmx86utils.a: No such file or directory c++: /obj/arm.arm/src/tmp/src/usr.bin/clang/clang/../../../lib/clang/libllvmcore/libllvmcore.a: No such file or directory *** Error code 1 Stop. make: stopped in /src/usr.bin/clang/clang *** Error code 1 Stop. make: stopped in /src/usr.bin/clang ===> usr.bin/clang/clang (install) sh /src/tools/install.sh -s -o root -g wheel -m 555 clang /obj/arm.arm/src/tmp/usr/bin/clang install: clang: No such file or directory *** Error code 71 Stop. make: stopped in /src/usr.bin/clang/clang *** Error code 1 Stop. make: stopped in /src/usr.bin/clang *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop. make: stopped in /src *** Error code 1 Stop in /src. TB --- 2013-06-22 00:46:29 - WARNING: /usr/bin/make returned exit code 1 TB --- 2013-06-22 00:46:29 - ERROR: failed to build world TB --- 2013-06-22 00:46:29 - 1373.73 user 148.95 system 1570.30 real http://tinderbox.freebsd.org/tinderbox-head-build-HEAD-arm-arm.full