From owner-freebsd-hackers@FreeBSD.ORG Sun May 10 12:53:53 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 453F2106566C for ; Sun, 10 May 2009 12:53:53 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: from mail-bw0-f165.google.com (mail-bw0-f165.google.com [209.85.218.165]) by mx1.freebsd.org (Postfix) with ESMTP id B6B428FC08 for ; Sun, 10 May 2009 12:53:52 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: by bwz9 with SMTP id 9so2162862bwz.43 for ; Sun, 10 May 2009 05:53:51 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:date:message-id:subject :from:to:content-type:content-transfer-encoding; bh=VTX6f9PjUZFL0WAkCH5mUkNtrTl8MT7aDmBHnL75hc8=; b=evLvi7xaHLV41x67JzmFZIM4BG8bNFwYg/I9+kPm8TS9SKpqr+LMNr8myeUqH3/3cN QonREWy0k00iVh8Ma03wwnXyTM/iay1xJzObMomFOuJdj09eTSbURzTWLFc8+WdSXAUX R+sQW//IgTg7ybRdgrEdxMY6ycHUVtod/CX/w= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:date:message-id:subject:from:to:content-type :content-transfer-encoding; b=X6UBW+5HltglxJaaw5v79nLZNm0Q5GZNg2aAXVCYAEtUC9xvfneskU7u+USZh6UH+7 860MOO7WNrnycjibvAb7BNj/rWCVIu7dHD+Xfmh9oaW1RgIG1FdzqvPieK7uBfPvshk8 AHoff+T3mG9U4zHwdN7IkvcEUxUpLtsr4ujNg= MIME-Version: 1.0 Received: by 10.239.143.138 with SMTP id k10mr346636hba.5.1241958777273; Sun, 10 May 2009 05:32:57 -0700 (PDT) Date: Sun, 10 May 2009 13:32:57 +0100 Message-ID: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> From: Ray Kinsella To: freebsd-hackers@freebsd.org Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Subject: contigmalloc & access protection failure X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 10 May 2009 12:53:53 -0000 Hi all, I am trying to create a kernel panic with a memory access volition, the memory I am allocating is physically contiguous and is 2 pages in size, I then try to use vm_map_protect to set the access flags of the 2nd page to disables writes, vm_map_protect returns successful but when I write to the page no access volition occurs, what am I missing? My attempt in source code to create the volition is below. Also a question about the FreeBSD memory manager, I am a bit confused, I read the source code of the vm_map_protect function and I see it sets the protection on a vm_map_entry_t, my expectation was protection would be set on vm_page_t, my understanding was this:- each vm_map_t contains 1 or more vm_map_entry_t each vm_map_entry_t contains 1 vm_object_t each vm_object_t contains 1 or more vm_page_t so does this mean that because protection is getting set at vm_map_entry, am I actually protecting more than one page of memory? Thanks Ray Kinsella --------------------------------------------- cut here --------------------------------------------- #include #include #include #include #include #include #include #include #include #include #include #include vm_offset_t palloc_wr; vm_offset_t palloc_r; void _alloc(void); void _free(void); void _alloc(void) { =A0=A0=A0 uint32_t retval =3D 0; =A0=A0=A0=A0 =A0=A0=A0 palloc_wr =3D (vm_offset_t) contigmalloc(2 * PAGE_SI= ZE, =A0=A0=A0 =A0=A0=A0 =A0=A0=A0 M_DEVBUF, 0, 0, (1L << 31), =A0=A0=A0 =A0=A0=A0 =A0=A0=A0 4096, 1024 * 1024); =A0=A0=A0 printf("contigmalloc : 0x%.08x\n", palloc_wr); =A0=A0=A0 palloc_r =3D palloc_wr + PAGE_SIZE; =A0=A0=A0 //kernel_map =A0=A0=A0 retval =3D vm_map_protect(&curthread->td_proc->p_vmspace->vm_map =A0=A0=A0 =A0=A0=A0 =A0=A0=A0 , palloc_r, palloc_r + PAGE_SIZE, =A0=A0=A0 =A0=A0=A0 =A0=A0=A0 VM_PROT_ALL, 0); =A0=A0=A0 printf("vm_map_protect : %d\n", retval); =A0=A0=A0 memset((void *)palloc_r,0xFF, PAGE_SIZE); } void _free(void) { =A0=A0=A0 contigfree((void *) palloc_wr, 2 * PAGE_SIZE, M_DEVBUF); } /* The function called at load/unload. */ static int event_handler(struct module *module, int event, void *arg) { =A0=A0=A0=A0=A0=A0=A0 int e =3D 0; /* Error, 0 for normal return status */ =A0=A0=A0=A0=A0=A0=A0 switch (event) { =A0=A0=A0=A0=A0=A0=A0 case MOD_LOAD: =A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0 _alloc(); =A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0 break; =A0=A0=A0=A0=A0=A0=A0 case MOD_UNLOAD: =A0=A0=A0 =A0=A0=A0 _free(); =A0=A0=A0 =A0=A0=A0 break; =A0=A0=A0=A0=A0=A0=A0 default: =A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0 e =3D EOPNOTSUPP; /* Error, O= peration Not Supported */ =A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0 break; =A0=A0=A0=A0=A0=A0=A0 } =A0=A0=A0=A0=A0=A0=A0 return(e); } /* The second argument of DECLARE_MODULE. */ static moduledata_t mod_conf =3D { =A0=A0=A0 "mod",=A0=A0=A0 /* module name */ =A0=A0=A0=A0 event_handler,=A0 /* event handler */ =A0=A0=A0=A0 NULL=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0=A0 /* extra data */ }; DECLARE_MODULE(mod, mod_conf, SI_SUB_DRIVERS, SI_ORDER_MIDDLE); From owner-freebsd-hackers@FreeBSD.ORG Sun May 10 13:37:57 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 378DE106566C for ; Sun, 10 May 2009 13:37:57 +0000 (UTC) (envelope-from rysto32@gmail.com) Received: from mail-bw0-f165.google.com (mail-bw0-f165.google.com [209.85.218.165]) by mx1.freebsd.org (Postfix) with ESMTP id B1A648FC08 for ; Sun, 10 May 2009 13:37:56 +0000 (UTC) (envelope-from rysto32@gmail.com) Received: by bwz9 with SMTP id 9so2174617bwz.43 for ; Sun, 10 May 2009 06:37:55 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type; bh=gpDrH7rlXjmjDzMpMT28IkvoFvtvB9WsT8XfANKwCCU=; b=d/aQDRe7QqcpH4b2AFw25DSR3WvxZPW8+ldfZYot7M2+SdFkoPJV6gjqsLxr5H6NxR WIVLDnnQxVSsogHJlS1ZzTHCY3XnJ9JuS3nuhqSSpBFF31Jr/j7PqqK9a85PuAkvEKLw z9BWk2/A6z9dZiuNY3fR+HbuBshwWrYPUu720= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; b=j1+4SXUWRhjJ4Q2O5umzYx00yk8kclM2RuT0pRjX8FEw105+z7zEVEK8DmpagRlo89 nEkAZxV7siVpf+Tsr8AQfm+JoHdKL8Y6Dzo5fxpTeWrjImPoRU/LMMmtCVHMHeB6slpI KG4fqKHiZ75SRtTXH6pjRO5M/DFoTIThqlR5Y= MIME-Version: 1.0 Received: by 10.239.150.9 with SMTP id l9mr333732hbb.147.1241962675623; Sun, 10 May 2009 06:37:55 -0700 (PDT) In-Reply-To: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> References: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> Date: Sun, 10 May 2009 09:37:55 -0400 Message-ID: From: Ryan Stone To: Ray Kinsella Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit X-Content-Filtered-By: Mailman/MimeDel 2.1.5 Cc: freebsd-hackers@freebsd.org Subject: Re: contigmalloc & access protection failure X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 10 May 2009 13:37:57 -0000 You're loading this through kldload? Then I'd imagine that curthread->td_proc->p_vmspace->vm_map refers to the vm_map of the kldload process, not the kernel. Try using kernel_map directly. Ryan Stone From owner-freebsd-hackers@FreeBSD.ORG Sun May 10 16:23:00 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id D5D87106564A for ; Sun, 10 May 2009 16:23:00 +0000 (UTC) (envelope-from rysto32@gmail.com) Received: from mail-bw0-f165.google.com (mail-bw0-f165.google.com [209.85.218.165]) by mx1.freebsd.org (Postfix) with ESMTP id 5F6D48FC12 for ; Sun, 10 May 2009 16:23:00 +0000 (UTC) (envelope-from rysto32@gmail.com) Received: by bwz9 with SMTP id 9so2222762bwz.43 for ; Sun, 10 May 2009 09:22:59 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type; bh=sza5QN3murGz7a89iRDvP+U55MzdHgsCo2YD2hSbL5U=; b=Xae14uJCXxv6NmVKjES81/4PHQWj5Pr2i0kwcNrvtzV0YDMENrMbZopfBHdkRjo9aj pugASRCba3Ark4eExU9BEueFNzqn1NvtbBL6mKrjNtEP37uWAjd03RsL23OEwmj7A7K8 MtXkb65+za3pYb0yaIshaZxkWuEVVBKW9eAEo= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type; b=VIIfNbNpYHpYoyPmWJqA81wyq+439N0aTbQgGehdu4O1B5CgXaIrpws8HYlKASM1+U vfdR3m0NK+6gY6+UGAXXqZUR02ZxMSL8hOVRIUH2xD3gvWgb3CLPrLQ/T27RAzP1NOWv nz6XZt+be/8F48B2BBA2a2JMFXbKpME51KXf8= MIME-Version: 1.0 Received: by 10.239.162.70 with SMTP id k6mr344403hbd.109.1241972579155; Sun, 10 May 2009 09:22:59 -0700 (PDT) In-Reply-To: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> References: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> Date: Sun, 10 May 2009 12:22:59 -0400 Message-ID: From: Ryan Stone To: Ray Kinsella Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit X-Content-Filtered-By: Mailman/MimeDel 2.1.5 Cc: freebsd-hackers@freebsd.org Subject: Re: contigmalloc & access protection failure X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 10 May 2009 16:23:01 -0000 Oh, and you're passing VM_PROT_ALL -- that says "map this read/write/execute". You want VM_PROT_READ Ryan Stone From owner-freebsd-hackers@FreeBSD.ORG Sun May 10 16:58:13 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 572C01065672 for ; Sun, 10 May 2009 16:58:13 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: from mail-fx0-f216.google.com (mail-fx0-f216.google.com [209.85.220.216]) by mx1.freebsd.org (Postfix) with ESMTP id DA7EB8FC19 for ; Sun, 10 May 2009 16:58:12 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: by fxm12 with SMTP id 12so2281386fxm.43 for ; Sun, 10 May 2009 09:58:12 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type :content-transfer-encoding; bh=0pu/FL8YEBnigkP/u+N4wmmxnXnGSuQ1UNKks70VIss=; b=ccWy/Re+HtEw4wTFNiBu9E7EpoxCreBwCMObdxh4zf34lV+KiWdo0zuL4RDLsjAKlO hVh1AjW4dcRyin1OzS57kn3QytgyxDzJa19prDyKf1tkuG2HfawVKmotoDgQOdPzX+cS gDn84oZLJ0+bjVbjs6Q6bab9HfblkyK68eQyk= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type:content-transfer-encoding; b=BCUwXc4902H3ODMaVX9/PpItZhjhyj/Sa2i6/ObBPbn9MgJYBw5xcMJZk5sl69ohPQ DzZNYqglGBw3A5Whh2n8H2RNimSu361Mcmmp3/JKaqkcjzK+LKjp92sWw8Y+xnIjseW1 CU1PFIwA6Uud2xMWwf/v1LxcjR6aE/IhcIuO8= MIME-Version: 1.0 Received: by 10.239.134.65 with SMTP id 1mr302646hby.160.1241974691943; Sun, 10 May 2009 09:58:11 -0700 (PDT) In-Reply-To: References: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> Date: Sun, 10 May 2009 17:58:11 +0100 Message-ID: <584ec6bb0905100958m1a0ee883h76eaa41eb566e033@mail.gmail.com> From: Ray Kinsella To: Ryan Stone Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org Subject: Re: contigmalloc & access protection failure X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 10 May 2009 16:58:13 -0000 ah I specified VM_PROT_ALL because I though that was "protecting" against reads/writes and executes. I had it the wrong way around, it was that VM_PROT that confused me, my kernel panic works perfectly now thanks. Regards Ray Kinsella On Sun, May 10, 2009 at 5:22 PM, Ryan Stone wrote: > Oh, and you're passing VM_PROT_ALL -- that says "map this > read/write/execute".=A0 You want VM_PROT_READ > > Ryan Stone > From owner-freebsd-hackers@FreeBSD.ORG Sun May 10 17:13:15 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 3C4D91065745 for ; Sun, 10 May 2009 17:13:15 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: from mail-bw0-f165.google.com (mail-bw0-f165.google.com [209.85.218.165]) by mx1.freebsd.org (Postfix) with ESMTP id B50AC8FC27 for ; Sun, 10 May 2009 17:13:14 +0000 (UTC) (envelope-from raykinsella78@gmail.com) Received: by bwz9 with SMTP id 9so2238951bwz.43 for ; Sun, 10 May 2009 10:13:13 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type :content-transfer-encoding; bh=foA065q2AG1QqQaQYEFprfZv2n6kP3rAfuodurNBp6E=; b=R4RK9yFgso5MmQz/KuvvJM3gPbNjZRr4dLL3woJCbZ0qoaumkN1bJ/Eaw6hwDQeAdv 9QHxxN9QaVuHWq89gGOkokcqj7CXH4kVUa7qdPNLUGx5WzST6jJ5EiHya4nGn20LZ41a uITxUYWU4UyiIxzLncYQcXpYmD6DUoofXyvOE= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type:content-transfer-encoding; b=Tlr5akYx3VYCOpsRnDIuzmFjrhdrZzUWdjK9+eyuXJzTRxWWRvG+nYPShAcByOkq8H Thz/chIavOf6ftnwEdiaO9SO2Og3wX4zsVI1PiNnfNolVX/qC3VnOBlr0cAikbdzuGI8 TlmlsBhINKDkBqYikygUpbgGLK2bXlEl+C3Js= MIME-Version: 1.0 Received: by 10.239.134.65 with SMTP id 1mr303258hby.160.1241975593506; Sun, 10 May 2009 10:13:13 -0700 (PDT) In-Reply-To: References: <584ec6bb0905100532n36ae97b1rc5e6e31c23bdb44b@mail.gmail.com> Date: Sun, 10 May 2009 18:13:13 +0100 Message-ID: <584ec6bb0905101013p4ee4c3daq68a50d5983d3382a@mail.gmail.com> From: Ray Kinsella To: Ryan Stone Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org Subject: Re: contigmalloc & access protection failure X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sun, 10 May 2009 17:13:15 -0000 Hi Ryan, One last thing, thanks for your help, Can you recommend any articles or books on developing with the FreeBSD virtually memory manager? Thanks Ray Kinsella On Sun, May 10, 2009 at 5:22 PM, Ryan Stone wrote: > Oh, and you're passing VM_PROT_ALL -- that says "map this > read/write/execute".=A0 You want VM_PROT_READ > > Ryan Stone > From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 10:06:04 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 63A84106566B for ; Mon, 11 May 2009 10:06:04 +0000 (UTC) (envelope-from brampton@gmail.com) Received: from mail-fx0-f216.google.com (mail-fx0-f216.google.com [209.85.220.216]) by mx1.freebsd.org (Postfix) with ESMTP id E958D8FC13 for ; Mon, 11 May 2009 10:06:03 +0000 (UTC) (envelope-from brampton@gmail.com) Received: by fxm12 with SMTP id 12so2586933fxm.43 for ; Mon, 11 May 2009 03:06:02 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:sender:received:in-reply-to :references:date:x-google-sender-auth:message-id:subject:from:to:cc :content-type:content-transfer-encoding; bh=EuywAZaTO0y8/uKfv5pBMDl2XZ1MDooMLPpi2Z6JnSI=; b=n5KGwBNKCNzz9oSZYc1BOBNluXm8yxBZjJ4mLeTCg1BBbC/O9wvjd2vaZpwYqCwAEP fAsIsl3tL8d0/OgPgl4P8flcD7G0mmM9QVykRizqCICXoesz+hEtVYnn54dMONgWO3Fw uxhjxq0NdT27XJyvJqSvwbARmL14v1Uu01WzI= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:sender:in-reply-to:references:date :x-google-sender-auth:message-id:subject:from:to:cc:content-type :content-transfer-encoding; b=HCTq7p1w0sLIr1CnIEM+AbWLoVAoTprJO1tahvCfQS10cTCTIRU6n3aIJWmOo4uzGR gzaYH3j+8VLnlS9E5hEK2tQJubf5faGo8KmazIjJ8206BnSYOckDQW9iMOakei5Gd8HF asVEdQ2J1LV6OozvxkH4a/OBZuD8K3DJoNpkw= MIME-Version: 1.0 Sender: brampton@gmail.com Received: by 10.223.103.133 with SMTP id k5mr3517571fao.23.1242036362643; Mon, 11 May 2009 03:06:02 -0700 (PDT) In-Reply-To: References: Date: Mon, 11 May 2009 11:06:02 +0100 X-Google-Sender-Auth: 32c470f204c16f2e Message-ID: From: Andrew Brampton To: freebsd-hackers@freebsd.org Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 7bit Cc: Ryan Stone Subject: Re: kthreads and sched_relinquish X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 10:06:04 -0000 2009/5/8 Ryan Stone : > Your kernel thread likely has a higher priority than userspace threads. > > Ryan Stone > Thanks for your reply Ryan. So that I understand this correctly, if I had two kernel threads, one with a high priority, and one with a low priority, and both are PRI_TIMESHARE, then the high priority thread will run uninterrupted until it sleeps? Or is it that kernel threads trumps userspace threads? >From my experience in userspace, all threads will get a chance to run, even if there is a higher priority thread ready to run. The exact problem I am having is that this code (written by someone else) has implemented their own spin locks (which of course does not sleep), so when the lower priority user thread obtains the lock, and higher priority thread sometimes gets rescheduled before the user thread has released the lock. Now the high priority thread spins forever waiting for it to be released, which doesn't seem to give the lower thread a chance. Of course the correct solution to this is to remove these custom built spin locks and start to use the locking mechanisms provided by FreeBSD. While I've started to do that, I wanted to explore this more for my general understanding. thanks Andrew From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 16:49:42 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 8325E1065676 for ; Mon, 11 May 2009 16:49:42 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 543118FC1E for ; Mon, 11 May 2009 16:49:42 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id 055EF46B8B; Mon, 11 May 2009 12:49:42 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id C2A2B8A025; Mon, 11 May 2009 12:49:40 -0400 (EDT) From: John Baldwin To: freebsd-hackers@freebsd.org Date: Mon, 11 May 2009 12:24:26 -0400 User-Agent: KMail/1.9.7 References: <20090508214117.GY58540@hoeg.nl> In-Reply-To: <20090508214117.GY58540@hoeg.nl> MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: 7bit Content-Disposition: inline Message-Id: <200905111224.26856.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Mon, 11 May 2009 12:49:40 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: Ed Schouten , jt@0xabadba.be, vasanth raonaik Subject: Re: concurrent sysctl implementation X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 16:49:42 -0000 On Friday 08 May 2009 5:41:17 pm Ed Schouten wrote: > A solution would be to solve it as follows: > > - Use a semaphore, initialized to some insane high value to put an upper > limit on the amount of concurrent sysctl calls. I'm not sure whether > this is really needed. Maybe this issue is not as serious as we think > it is. Well, one compromise might be to allow concurrent userland requests if the buffer size is small (say < 1 page). This would be a quite simple change and would cover many common syscalls like fetching an int which don't wire memory anyway. > - Use an rw/rm/sxlock to protect the sysctl tree, but only pick up > the lock when we traverse parts of the sysctl tree that has > dynamically created entries. I don't think further work is needed here for the tree, notice that in-kernel sysctls are already concurrent and use a read lock on the tree. -- John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 18:25:07 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id C7FEC106566C for ; Mon, 11 May 2009 18:25:07 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 9BF588FC16 for ; Mon, 11 May 2009 18:25:07 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id 31A0346B7E; Mon, 11 May 2009 14:25:07 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id AECFF8A025; Mon, 11 May 2009 14:25:05 -0400 (EDT) From: John Baldwin To: freebsd-hackers@freebsd.org Date: Mon, 11 May 2009 14:05:07 -0400 User-Agent: KMail/1.9.7 References: <46FDBAFC.1010000@gmail.com> In-Reply-To: <46FDBAFC.1010000@gmail.com> MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: 7bit Content-Disposition: inline Message-Id: <200905111405.07289.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Mon, 11 May 2009 14:25:05 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 18:25:08 -0000 On Friday 28 September 2007 10:39:56 pm Ighighi wrote: > The POXIX prototype for readlink(2) is: > ssize_t readlink(const char *restrict path, char *restrict buf, size_t > bufsize); It can't simply be corrected as it would change the ABI and thus requires a new system call, etc. However, do you really expect a symlink to be longer than 2^31 on a 64-bit machine? -- John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 18:28:10 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0976A1065672 for ; Mon, 11 May 2009 18:28:10 +0000 (UTC) (envelope-from jt@0xabadba.be) Received: from ey-out-2122.google.com (ey-out-2122.google.com [74.125.78.26]) by mx1.freebsd.org (Postfix) with ESMTP id 7312C8FC0C for ; Mon, 11 May 2009 18:28:09 +0000 (UTC) (envelope-from jt@0xabadba.be) Received: by ey-out-2122.google.com with SMTP id 9so913789eyd.7 for ; Mon, 11 May 2009 11:28:08 -0700 (PDT) MIME-Version: 1.0 Received: by 10.216.19.198 with SMTP id n48mr3577774wen.41.1242066488158; Mon, 11 May 2009 11:28:08 -0700 (PDT) X-Originating-IP: [192.52.218.45] In-Reply-To: <200905111224.26856.jhb@freebsd.org> References: <20090508214117.GY58540@hoeg.nl> <200905111224.26856.jhb@freebsd.org> From: jt@0xabadba.be Date: Mon, 11 May 2009 14:27:48 -0400 Message-ID: To: John Baldwin Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org Subject: Re: concurrent sysctl implementation X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 18:28:10 -0000 John, Thank you for your input on this matter, I'm excited to write some software for this project since its given me great code to learn from as i've grown up (still a kid though :). My questions are a bit more detailed below. On Mon, May 11, 2009 at 12:24 PM, John Baldwin wrote: > On Friday 08 May 2009 5:41:17 pm Ed Schouten wrote: >> A solution would be to solve it as follows: >> >> - Use a semaphore, initialized to some insane high value to put an upper >> =A0 limit on the amount of concurrent sysctl calls. I'm not sure whether >> =A0 this is really needed. Maybe this issue is not as serious as we thin= k >> =A0 it is. > > Well, one compromise might be to allow concurrent userland requests if th= e > buffer size is small (say < 1 page). =A0This would be a quite simple chan= ge and > would cover many common syscalls like fetching an int which don't wire me= mory > anyway. Why is this a compromise? Isn't concurrent sysctl calls from userland a good thing? What materials would be good to read other than the code and the sysctl manual pages? You said it would be relatively easy to implement this; what methods should I be considering to do this in and what part of the code specifically should I be looking at? > >> - Use an rw/rm/sxlock to protect the sysctl tree, but only pick up >> =A0 the lock when we traverse parts of the sysctl tree that has >> =A0 dynamically created entries. > > I don't think further work is needed here for the tree, notice that in-ke= rnel > sysctls are already concurrent and use a read lock on the tree. yes i've seen the locking mechanism, it reminds me of a monitor type system... though from my understanding monitors appear seldom compared to semaphores in the kernel. I assume the lock will need a bit of twiddling with in some areas of the code if I'm going to enable concurrency from userland, when its said that we should consider the things that are dynamic would it be better to implement this with more than one "queue" or list? Instead perhaps break them up into several lists or, more fundamentally, two lists -- those that are dynamically created entries and those that are not -- is this even feasible to distinguish between the two originally and then on the fly later? Thanks a lot! Respectfully, /jt From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 18:33:15 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0BEBD1065689; Mon, 11 May 2009 18:33:15 +0000 (UTC) (envelope-from kostikbel@gmail.com) Received: from mail.terabit.net.ua (mail.terabit.net.ua [195.137.202.147]) by mx1.freebsd.org (Postfix) with ESMTP id A0D1E8FC1D; Mon, 11 May 2009 18:33:14 +0000 (UTC) (envelope-from kostikbel@gmail.com) Received: from skuns.zoral.com.ua ([91.193.166.194] helo=mail.zoral.com.ua) by mail.terabit.net.ua with esmtps (TLSv1:AES256-SHA:256) (Exim 4.63 (FreeBSD)) (envelope-from ) id 1M3aJL-000A2l-Us; Mon, 11 May 2009 21:33:12 +0300 Received: from deviant.kiev.zoral.com.ua (root@deviant.kiev.zoral.com.ua [10.1.1.148]) by mail.zoral.com.ua (8.14.2/8.14.2) with ESMTP id n4BIX9Kf025962 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Mon, 11 May 2009 21:33:09 +0300 (EEST) (envelope-from kostikbel@gmail.com) Received: from deviant.kiev.zoral.com.ua (kostik@localhost [127.0.0.1]) by deviant.kiev.zoral.com.ua (8.14.3/8.14.3) with ESMTP id n4BIX9i3082703; Mon, 11 May 2009 21:33:09 +0300 (EEST) (envelope-from kostikbel@gmail.com) Received: (from kostik@localhost) by deviant.kiev.zoral.com.ua (8.14.3/8.14.3/Submit) id n4BIX9Dc082702; Mon, 11 May 2009 21:33:09 +0300 (EEST) (envelope-from kostikbel@gmail.com) X-Authentication-Warning: deviant.kiev.zoral.com.ua: kostik set sender to kostikbel@gmail.com using -f Date: Mon, 11 May 2009 21:33:09 +0300 From: Kostik Belousov To: John Baldwin Message-ID: <20090511183309.GB1948@deviant.kiev.zoral.com.ua> References: <46FDBAFC.1010000@gmail.com> <200905111405.07289.jhb@freebsd.org> Mime-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="ePr0Yc6hYRI4V1o7" Content-Disposition: inline In-Reply-To: <200905111405.07289.jhb@freebsd.org> User-Agent: Mutt/1.4.2.3i X-Virus-Scanned: ClamAV version 0.94.2, clamav-milter version 0.94.2 on skuns.kiev.zoral.com.ua X-Virus-Status: Clean X-Spam-Status: No, score=-4.4 required=5.0 tests=ALL_TRUSTED,AWL,BAYES_00 autolearn=ham version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on skuns.kiev.zoral.com.ua X-Virus-Scanned: mail.terabit.net.ua 1M3aJL-000A2l-Us 6cecd4be097efb670a57f2fdda462b57 X-Terabit: YES Cc: freebsd-hackers@freebsd.org, Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 18:33:15 -0000 --ePr0Yc6hYRI4V1o7 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable On Mon, May 11, 2009 at 02:05:07PM -0400, John Baldwin wrote: > On Friday 28 September 2007 10:39:56 pm Ighighi wrote: ^^^^^ > > The POXIX prototype for readlink(2) is: > > ssize_t readlink(const char *restrict path, char *restrict buf, size_t= =20 > > bufsize); >=20 > It can't simply be corrected as it would change the ABI and thus requires= a=20 > new system call, etc. However, do you really expect a symlink to be long= er=20 > than 2^31 on a 64-bit machine? Yes, I agree that this is ABI change. Meantime, r176215 | ru | 2008-02-12 22:09:04 +0200 (Tue, 12 Feb 2008) | 5 lines Change readlink(2)'s return type and type of the last argument to match POSIX. Prodded by: Alexey Lyashkov I tried to convince ru@ that ABI breakage is not good, but has not succeeded. --ePr0Yc6hYRI4V1o7 Content-Type: application/pgp-signature Content-Disposition: inline -----BEGIN PGP SIGNATURE----- Version: GnuPG v1.4.9 (FreeBSD) iEYEARECAAYFAkoIb2QACgkQC3+MBN1Mb4hpRwCg2ggUNA/xgcwRe77a3JDC1Tpo ujAAoJfdxAavXEegNUAE2gteoeOlzzgh =JLt3 -----END PGP SIGNATURE----- --ePr0Yc6hYRI4V1o7-- From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 18:46:21 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 64D98106566C; Mon, 11 May 2009 18:46:21 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 346738FC08; Mon, 11 May 2009 18:46:21 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id D972046B09; Mon, 11 May 2009 14:46:20 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id 912C28A026; Mon, 11 May 2009 14:46:19 -0400 (EDT) From: John Baldwin To: Kostik Belousov Date: Mon, 11 May 2009 14:46:14 -0400 User-Agent: KMail/1.9.7 References: <46FDBAFC.1010000@gmail.com> <200905111405.07289.jhb@freebsd.org> <20090511183309.GB1948@deviant.kiev.zoral.com.ua> In-Reply-To: <20090511183309.GB1948@deviant.kiev.zoral.com.ua> MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: 7bit Content-Disposition: inline Message-Id: <200905111446.14439.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Mon, 11 May 2009 14:46:19 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: freebsd-hackers@freebsd.org, Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 18:46:21 -0000 On Monday 11 May 2009 2:33:09 pm Kostik Belousov wrote: > On Mon, May 11, 2009 at 02:05:07PM -0400, John Baldwin wrote: > > On Friday 28 September 2007 10:39:56 pm Ighighi wrote: > ^^^^^ Yes, I had this stuck in the back of my head from when it first appeared. > > > The POXIX prototype for readlink(2) is: > > > ssize_t readlink(const char *restrict path, char *restrict buf, size_t > > > bufsize); > > > > It can't simply be corrected as it would change the ABI and thus requires a > > new system call, etc. However, do you really expect a symlink to be longer > > than 2^31 on a 64-bit machine? > > Yes, I agree that this is ABI change. > > Meantime, > r176215 | ru | 2008-02-12 22:09:04 +0200 (Tue, 12 Feb 2008) | 5 lines > > Change readlink(2)'s return type and type of the last argument > to match POSIX. > > Prodded by: Alexey Lyashkov > > I tried to convince ru@ that ABI breakage is not good, but has not > succeeded. Ugh, is this only in HEAD? If so, I will back it out for 8.0. If this made it into a release then this is a far bigger mess. Oh, good, this is only in 8. I will fix this ASAP. I can just add the new syscall I guess. -- John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 18:58:19 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id D945E1065673; Mon, 11 May 2009 18:58:19 +0000 (UTC) (envelope-from kostikbel@gmail.com) Received: from mail.terabit.net.ua (mail.terabit.net.ua [195.137.202.147]) by mx1.freebsd.org (Postfix) with ESMTP id 78C788FC08; Mon, 11 May 2009 18:58:19 +0000 (UTC) (envelope-from kostikbel@gmail.com) Received: from skuns.zoral.com.ua ([91.193.166.194] helo=mail.zoral.com.ua) by mail.terabit.net.ua with esmtps (TLSv1:AES256-SHA:256) (Exim 4.63 (FreeBSD)) (envelope-from ) id 1M3ahd-000F4H-Ub; Mon, 11 May 2009 21:58:17 +0300 Received: from deviant.kiev.zoral.com.ua (root@deviant.kiev.zoral.com.ua [10.1.1.148]) by mail.zoral.com.ua (8.14.2/8.14.2) with ESMTP id n4BIwFgc027346 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Mon, 11 May 2009 21:58:15 +0300 (EEST) (envelope-from kostikbel@gmail.com) Received: from deviant.kiev.zoral.com.ua (kostik@localhost [127.0.0.1]) by deviant.kiev.zoral.com.ua (8.14.3/8.14.3) with ESMTP id n4BIwFA9082936; Mon, 11 May 2009 21:58:15 +0300 (EEST) (envelope-from kostikbel@gmail.com) Received: (from kostik@localhost) by deviant.kiev.zoral.com.ua (8.14.3/8.14.3/Submit) id n4BIwEtk082935; Mon, 11 May 2009 21:58:14 +0300 (EEST) (envelope-from kostikbel@gmail.com) X-Authentication-Warning: deviant.kiev.zoral.com.ua: kostik set sender to kostikbel@gmail.com using -f Date: Mon, 11 May 2009 21:58:14 +0300 From: Kostik Belousov To: John Baldwin Message-ID: <20090511185814.GD1948@deviant.kiev.zoral.com.ua> References: <46FDBAFC.1010000@gmail.com> <200905111405.07289.jhb@freebsd.org> <20090511183309.GB1948@deviant.kiev.zoral.com.ua> <200905111446.14439.jhb@freebsd.org> Mime-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="8nuB+PMTZvqSz3PP" Content-Disposition: inline In-Reply-To: <200905111446.14439.jhb@freebsd.org> User-Agent: Mutt/1.4.2.3i X-Virus-Scanned: ClamAV version 0.94.2, clamav-milter version 0.94.2 on skuns.kiev.zoral.com.ua X-Virus-Status: Clean X-Spam-Status: No, score=-4.4 required=5.0 tests=ALL_TRUSTED,AWL,BAYES_00 autolearn=ham version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on skuns.kiev.zoral.com.ua X-Virus-Scanned: mail.terabit.net.ua 1M3ahd-000F4H-Ub 3ac93a7942003afc1726dc909ec4642c X-Terabit: YES Cc: freebsd-hackers@freebsd.org, Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 18:58:20 -0000 --8nuB+PMTZvqSz3PP Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable On Mon, May 11, 2009 at 02:46:14PM -0400, John Baldwin wrote: > On Monday 11 May 2009 2:33:09 pm Kostik Belousov wrote: > > On Mon, May 11, 2009 at 02:05:07PM -0400, John Baldwin wrote: > > > On Friday 28 September 2007 10:39:56 pm Ighighi wrote: > > ^^^^^ >=20 > Yes, I had this stuck in the back of my head from when it first appeared. >=20 > > > > The POXIX prototype for readlink(2) is: > > > > ssize_t readlink(const char *restrict path, char *restrict buf, siz= e_t=20 > > > > bufsize); > > >=20 > > > It can't simply be corrected as it would change the ABI and thus requ= ires=20 > a=20 > > > new system call, etc. However, do you really expect a symlink to be= =20 > longer=20 > > > than 2^31 on a 64-bit machine? > >=20 > > Yes, I agree that this is ABI change. > >=20 > > Meantime, > > r176215 | ru | 2008-02-12 22:09:04 +0200 (Tue, 12 Feb 2008) | 5 lines > >=20 > > Change readlink(2)'s return type and type of the last argument > > to match POSIX. > >=20 > > Prodded by: Alexey Lyashkov > >=20 > > I tried to convince ru@ that ABI breakage is not good, but has not > > succeeded. >=20 > Ugh, is this only in HEAD? If so, I will back it out for 8.0. If this m= ade=20 > it into a release then this is a far bigger mess. Oh, good, this is only= in=20 > 8. I will fix this ASAP. I can just add the new syscall I guess. You need to symver the syscalls. It requires some ugly games with our syscall stubs, because gnu ld only honor .symver in the same object where the symbol is defined. I did prototyped this some time ago, by including a file with appropriate .symver from all stubs. --8nuB+PMTZvqSz3PP Content-Type: application/pgp-signature Content-Disposition: inline -----BEGIN PGP SIGNATURE----- Version: GnuPG v1.4.9 (FreeBSD) iEYEARECAAYFAkoIdUYACgkQC3+MBN1Mb4ifzACgrLpVJ3GBpJiibydOVyKaPbZY v/YAnAo8BjIyRA0+wApIBZong+B3aHWf =7S0J -----END PGP SIGNATURE----- --8nuB+PMTZvqSz3PP-- From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 22:14:26 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 505081065673; Mon, 11 May 2009 22:14:26 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 21E218FC0A; Mon, 11 May 2009 22:14:26 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id CB47946B09; Mon, 11 May 2009 18:14:25 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id B107C8A025; Mon, 11 May 2009 18:14:24 -0400 (EDT) From: John Baldwin To: Kostik Belousov Date: Mon, 11 May 2009 16:23:52 -0400 User-Agent: KMail/1.9.7 References: <46FDBAFC.1010000@gmail.com> <200905111446.14439.jhb@freebsd.org> <20090511185814.GD1948@deviant.kiev.zoral.com.ua> In-Reply-To: <20090511185814.GD1948@deviant.kiev.zoral.com.ua> MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: 7bit Content-Disposition: inline Message-Id: <200905111623.52881.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Mon, 11 May 2009 18:14:24 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: freebsd-hackers@freebsd.org, Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 22:14:26 -0000 On Monday 11 May 2009 2:58:14 pm Kostik Belousov wrote: > On Mon, May 11, 2009 at 02:46:14PM -0400, John Baldwin wrote: > > On Monday 11 May 2009 2:33:09 pm Kostik Belousov wrote: > > > On Mon, May 11, 2009 at 02:05:07PM -0400, John Baldwin wrote: > > > > On Friday 28 September 2007 10:39:56 pm Ighighi wrote: > > > ^^^^^ > > > > Yes, I had this stuck in the back of my head from when it first appeared. > > > > > > > The POXIX prototype for readlink(2) is: > > > > > ssize_t readlink(const char *restrict path, char *restrict buf, size_t > > > > > bufsize); > > > > > > > > It can't simply be corrected as it would change the ABI and thus requires > > a > > > > new system call, etc. However, do you really expect a symlink to be > > longer > > > > than 2^31 on a 64-bit machine? > > > > > > Yes, I agree that this is ABI change. > > > > > > Meantime, > > > r176215 | ru | 2008-02-12 22:09:04 +0200 (Tue, 12 Feb 2008) | 5 lines > > > > > > Change readlink(2)'s return type and type of the last argument > > > to match POSIX. > > > > > > Prodded by: Alexey Lyashkov > > > > > > I tried to convince ru@ that ABI breakage is not good, but has not > > > succeeded. > > > > Ugh, is this only in HEAD? If so, I will back it out for 8.0. If this made > > it into a release then this is a far bigger mess. Oh, good, this is only in > > 8. I will fix this ASAP. I can just add the new syscall I guess. > > You need to symver the syscalls. It requires some ugly games with our > syscall stubs, because gnu ld only honor .symver in the same object where > the symbol is defined. I did prototyped this some time ago, by including > a file with appropriate .symver from all stubs. So, after thinking about this out loud some more, it seems the ABI breakage would only be for 64-bit platforms that passed a -ve value as the buffer size. However, doing so would already either panic due to triggering an assertion, or result in otherwise undefined behavior and that making the new parameter unsigned actually results in the same undefined behavior in the non-panic case. -- John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Mon May 11 22:14:27 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 73421106566B for ; Mon, 11 May 2009 22:14:27 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 37DB88FC0C for ; Mon, 11 May 2009 22:14:27 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id D9B8846B0D; Mon, 11 May 2009 18:14:26 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id 9541B8A026; Mon, 11 May 2009 18:14:25 -0400 (EDT) From: John Baldwin To: jt@0xabadba.be Date: Mon, 11 May 2009 18:01:18 -0400 User-Agent: KMail/1.9.7 References: <200905111224.26856.jhb@freebsd.org> In-Reply-To: MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: quoted-printable Content-Disposition: inline Message-Id: <200905111801.18767.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Mon, 11 May 2009 18:14:25 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: freebsd-hackers@freebsd.org Subject: Re: concurrent sysctl implementation X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Mon, 11 May 2009 22:14:27 -0000 On Monday 11 May 2009 2:27:48 pm jt@0xabadba.be wrote: > John, >=20 > Thank you for your input on this matter, I'm excited to write > some software for this project since its given me great code to learn > from as i've grown up (still a kid though :). My questions are a bit > more detailed below. >=20 > On Mon, May 11, 2009 at 12:24 PM, John Baldwin wrote: > > On Friday 08 May 2009 5:41:17 pm Ed Schouten wrote: > >> A solution would be to solve it as follows: > >> > >> - Use a semaphore, initialized to some insane high value to put an upp= er > >> =A0 limit on the amount of concurrent sysctl calls. I'm not sure wheth= er > >> =A0 this is really needed. Maybe this issue is not as serious as we th= ink > >> =A0 it is. > > > > Well, one compromise might be to allow concurrent userland requests if = the > > buffer size is small (say < 1 page). =A0This would be a quite simple ch= ange=20 and > > would cover many common syscalls like fetching an int which don't wire= =20 memory > > anyway. >=20 > Why is this a compromise? Isn't concurrent sysctl calls from userland > a good thing? What materials would be good to read other than the > code and the sysctl manual pages? You said it would be relatively > easy to implement this; what methods should I be considering to do > this in and what part of the code specifically should I be looking at? Well, in theory a bunch of "small" requests to SYSCTL_PROC() nodes that use= d=20 sysctl_wire_old() (or whatever it is called) could cause the amount of user= =20 memory wired for sysctls to grow unbounded. Thus, allowing this limited=20 concurrency is a tradeoff as there is a minimal (perhaps only theoretical a= t=20 the moment) risk of removing the safety net. The patch is quite small, btw, because the locking for the sysctl tree alre= ady=20 exists, and by using read locks, one can already allow concurrent sysctl=20 requests. There is no need to add any new locks or restructure the sysctl= =20 tree, just to adjust the locking that is already present. It might be=20 clearer, in fact, to split the sysctl memory lock back out into a separate= =20 lock. This would allow "small" sysctl requests to run concurrently with a= =20 single "large" request whereas in my suggestion in the earlier e-mail,=20 the "large" request will block all other user requests until it finishes. I've actually gone ahead and done this below. =2D-- //depot/projects/smpng/sys/kern/kern_sysctl.c 2009/05/08 11:53:25 +++ //depot/user/jhb/lock/kern/kern_sysctl.c 2009/05/11 21:58:08 @@ -77,11 +77,12 @@ * API rather than using the dynamic API. Use of the dynamic API is * strongly encouraged for most code. * =2D * This lock is also used to serialize userland sysctl requests. Some =2D * sysctls wire user memory, and serializing the requests limits the =2D * amount of wired user memory in use. + * The sysctlmemlock is used to limit the amount of user memory wired for + * sysctl requests. This is implemented by serializing any userland + * sysctl requests larger than a single page via an exclusive lock. */ static struct sx sysctllock; +static struct sx sysctlmemlock; =20 #define SYSCTL_SLOCK() sx_slock(&sysctllock) #define SYSCTL_SUNLOCK() sx_sunlock(&sysctllock) @@ -543,6 +544,7 @@ { struct sysctl_oid **oidp; =20 + sx_init(&sysctlmemlock, "sysctl mem"); SYSCTL_INIT(); SYSCTL_XLOCK(); SET_FOREACH(oidp, sysctl_set) @@ -1563,7 +1565,7 @@ size_t *oldlenp, int inkernel, void *new, size_t newlen, size_t *retva= l, int flags) { =2D int error =3D 0; + int error =3D 0, memlocked; struct sysctl_req req; =20 bzero(&req, sizeof req); @@ -1603,14 +1605,20 @@ if (KTRPOINT(curthread, KTR_SYSCTL)) ktrsysctl(name, namelen); #endif =2D=09 =2D SYSCTL_XLOCK(); + + if (req.oldlen > PAGE_SIZE) { + memlocked =3D 1; + sx_xlock(&sysctlmemlock); + } else + memlocked =3D 0; CURVNET_SET(TD_TO_VNET(curthread)); =20 for (;;) { req.oldidx =3D 0; req.newidx =3D 0; + SYSCTL_SLOCK(); error =3D sysctl_root(0, name, namelen, &req); + SYSCTL_SUNLOCK(); if (error !=3D EAGAIN) break; uio_yield(); @@ -1620,7 +1628,8 @@ =20 if (req.lock =3D=3D REQ_WIRED && req.validlen > 0) vsunlock(req.oldptr, req.validlen); =2D SYSCTL_XUNLOCK(); + if (memlocked) + sx_xunlock(&sysctlmemlock); =20 if (error && error !=3D ENOMEM) return (error); =2D-=20 John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Tue May 12 06:27:35 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0DDAD106566C for ; Tue, 12 May 2009 06:27:35 +0000 (UTC) (envelope-from to.my.trociny@gmail.com) Received: from mail-ew0-f207.google.com (mail-ew0-f207.google.com [209.85.219.207]) by mx1.freebsd.org (Postfix) with ESMTP id 95C5C8FC1F for ; Tue, 12 May 2009 06:27:34 +0000 (UTC) (envelope-from to.my.trociny@gmail.com) Received: by ewy3 with SMTP id 3so3945420ewy.43 for ; Mon, 11 May 2009 23:27:33 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:received:received:to:subject:organization:from :date:message-id:user-agent:mime-version:content-type; bh=2K1mssUc37Rx+3Tr2D8wq9uu2Nc5NozJYg/7OaZAKWc=; b=v1uGnzMGuYpuJ76vkQKwp3MRKYApBmM13wYwwxAY8DPPRTZQrw4qiDUD6DDFohoL64 Vj3O3eD690zsYWtazK8KqLuvmLK0JrfpjlcSm64+nI12eiRKynofi3yyRj/MHtQT1Djh ToJgcCj4F2EvGyM7PZ2CQgSQY5VgHAZ8kR+9w= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=to:subject:organization:from:date:message-id:user-agent :mime-version:content-type; b=mAusIMAAqD96/GkV3UMY6+esvs0FCZa8C1WhdPhvKbf4nzLmllG16kTbsm3ovzOpFO yt+vpLduJZ8rO79pAhjqy3pWEjMLwAHjUe6KSUBQmURg/86R/vfxC/i//0qW7D9zw7cV HcRddwJrarvDsGqqOoHdVjcGrR+v7n497LcMQ= Received: by 10.210.19.7 with SMTP id 7mr6235350ebs.37.1242109653621; Mon, 11 May 2009 23:27:33 -0700 (PDT) Received: from localhost (ms.singlescrowd.net [80.85.90.67]) by mx.google.com with ESMTPS id 23sm2933328eya.19.2009.05.11.23.27.32 (version=TLSv1/SSLv3 cipher=RC4-MD5); Mon, 11 May 2009 23:27:33 -0700 (PDT) To: freebsd-hackers@freebsd.org Organization: TOA Ukraine From: Mikolaj Golub Date: Tue, 12 May 2009 09:27:30 +0300 Message-ID: <814ovqn8dp.fsf@zhuzha.ua1> User-Agent: Gnus/5.11 (Gnus v5.11) Emacs/22.3 (berkeley-unix) MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Subject: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 12 May 2009 06:27:35 -0000 Hi, The code below is compiled with -fopenmp and run on FreeBSD6/7 (i386, amd64): #include #include int n = 4, m = 2; int main () { for (;;) { int i; //sleep(2); #pragma omp parallel for num_threads(m) for(i = 0; i < 1; i++) {} //sleep(2); #pragma omp parallel for num_threads(n) for(i = 0; i < 1; i++) {} } return 0; } During the run the program's virtual memory usage constantly grows. The growth is observed only when n != m. When running the program with uncommented sleep() and observing the number of threads with 'top -H' I see in turn 2 or 4 threads. So it looks like memory leak when thread is removed. Should I fill PR? -- Mikolaj Golub From owner-freebsd-hackers@FreeBSD.ORG Tue May 12 06:46:23 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id DC91E1065672 for ; Tue, 12 May 2009 06:46:23 +0000 (UTC) (envelope-from James.McPherson@Sun.COM) Received: from sineb-mail-1.sun.com (sineb-mail-1.sun.com [192.18.19.6]) by mx1.freebsd.org (Postfix) with ESMTP id 5DE5B8FC19 for ; Tue, 12 May 2009 06:46:23 +0000 (UTC) (envelope-from James.McPherson@Sun.COM) Received: from fe-apac-05.sun.com (fe-apac-05.sun.com [192.18.19.176] (may be forged)) by sineb-mail-1.sun.com (8.13.6+Sun/8.12.9) with ESMTP id n4C6k9EE007067 for ; Tue, 12 May 2009 06:46:22 GMT MIME-version: 1.0 Content-transfer-encoding: 7BIT Content-type: text/plain; charset=US-ASCII Received: from conversion-daemon.mail-apac.sun.com by mail-apac.sun.com (Sun Java(tm) System Messaging Server 7.0-5.01 64bit (built Feb 19 2009)) id <0KJI00B00QL4IL00@mail-apac.sun.com> for hackers@freebsd.org; Tue, 12 May 2009 14:46:09 +0800 (SGT) Received: from blinder ([unknown] [220.157.71.44]) by mail-apac.sun.com (Sun Java(tm) System Messaging Server 7.0-5.01 64bit (built Feb 19 2009)) with ESMTPSA id <0KJI003CUQSLBBB0@mail-apac.sun.com>; Tue, 12 May 2009 14:46:09 +0800 (SGT) Date: Tue, 12 May 2009 16:45:49 +1000 From: "James C. McPherson" Sender: James.McPherson@Sun.COM To: Undisclosed recipients: ; Message-id: <20090512164549.000011a9@blinder> Organization: Sun Microsystems X-Mailer: Claws Mail 3.7.0 (GTK+ 2.14.5; i386-pc-solaris2.11) X-Mailman-Approved-At: Tue, 12 May 2009 11:24:50 +0000 Subject: Kernel Conference Australia 2009 - registrations and agenda pages NOW LIVE X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 12 May 2009 06:46:24 -0000 Dear friends, It gives me great pleasure to announce that registrations for Kernel Conference Australia 2009 are now open, at http://au.sun.com/sunnews/events/2009/kernel/ The confirmed agenda and the speaker bio pages are here: http://au.sun.com/sunnews/events/2009/kernel/agenda.jsp http://au.sun.com/sunnews/events/2009/kernel/speakers.jsp I'm looking forward to seeing you there. James C. McPherson -- Senior Kernel Software Engineer, Solaris Sun Microsystems http://blogs.sun.com/jmcp http://www.jmcp.homeunix.com/blog Kernel Conference Australia - http://au.sun.com/sunnews/events/2009/kernel From owner-freebsd-hackers@FreeBSD.ORG Tue May 12 18:54:36 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 2171E1065677 for ; Tue, 12 May 2009 18:54:36 +0000 (UTC) (envelope-from rwatson@FreeBSD.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id F08528FC27 for ; Tue, 12 May 2009 18:54:35 +0000 (UTC) (envelope-from rwatson@FreeBSD.org) Received: from fledge.watson.org (fledge.watson.org [65.122.17.41]) by cyrus.watson.org (Postfix) with ESMTPS id B0B1A46B8D; Tue, 12 May 2009 14:54:35 -0400 (EDT) Date: Tue, 12 May 2009 19:54:35 +0100 (BST) From: Robert Watson X-X-Sender: robert@fledge.watson.org To: Konrad Heuer In-Reply-To: <20090508101555.J47014@gwdu60.gwdg.de> Message-ID: References: <20090508101555.J47014@gwdu60.gwdg.de> User-Agent: Alpine 2.00 (BSF 1167 2008-08-23) MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed Cc: freebsd-hackers@freebsd.org Subject: Re: How to invalidate NFS read cache? X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 12 May 2009 18:54:36 -0000 On Fri, 8 May 2009, Konrad Heuer wrote: > sporadically, I observe a strange but serious problem in our large NFS > environment. NFS servers are Linux and OS X with StorNext/Xsan cluster > filesystems, NFS clients Linux and FreeBSD. > > NFS client A changes a file, but nfs client B (running on FreeBSD) does > still see the old version. On the NFS server itself, everything looks fine. > > Afaik the FreeBSD kernel invalidates the NFS read cache if file modification > time on the server changed which should happen here but doesn't. Can I force > FreeBSD (e.g. by sysctl setting) to read file buffers again unconditionally > after vfs.nfs.access_cache_timeout seconds have passed? Hi Konrad: Normally, NFS clients implement open-to-close consistency, which dictates that when a close() occurs on client A, all pending writes on the file should be issued to the server before close() returns, so that a signal to client B to open() the file can validate its cache before open() returns. This raises the following question: is client A closing the file, and is client B then opening it? If not: relying on writes being visible on the client B before the close() on A and a fresh open() on B is not guaranteed to work, although we can discuss ways to improve behavior with respect to expectation. Try modifying your application and see if it gets the desired behavior, and then we can discuss ways to improve what you're seeing. If you are: this is probably a bug in our caching and or issuing of NFS RPCs. We cache both attribute and access data -- perhaps there is an open() path where we issue neither RPC? In the case of open, we likely should test for a valid access cache entry, and if there is one, issue an attribute read, and otherwise just issue an access check which will piggyback fresh attribute data on the reply. Perhaps there is a bug here somewhere. A few other misc questions: - Could you confirm you're using NFSv3 on all clients. Are there any special mount options in use? - What version of FreeBSD are you running with? In FreeBSD 8.x, we now have DTrace probes for all of the above events -- VOPs, attribute cache hit/miss/load/flush, access cache hit/miss/load/flush, RPCs, etc, which we can use to debug the problem. I haven't yet MFC'd these to 7.x, but if you're able to run a very fresh 7-STABLE, I can probably produce a patch to add it for you in a few days. Robert N M Watson Computer Laboratory University of Cambridge From owner-freebsd-hackers@FreeBSD.ORG Tue May 12 20:56:13 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id A0ED0106564A for ; Tue, 12 May 2009 20:56:13 +0000 (UTC) (envelope-from rwatson@FreeBSD.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 67A278FC15 for ; Tue, 12 May 2009 20:56:13 +0000 (UTC) (envelope-from rwatson@FreeBSD.org) Received: from fledge.watson.org (fledge.watson.org [65.122.17.41]) by cyrus.watson.org (Postfix) with ESMTPS id 9B39A46B65; Tue, 12 May 2009 16:56:12 -0400 (EDT) Date: Tue, 12 May 2009 21:56:12 +0100 (BST) From: Robert Watson X-X-Sender: robert@fledge.watson.org To: Konrad Heuer In-Reply-To: Message-ID: References: <20090508101555.J47014@gwdu60.gwdg.de> User-Agent: Alpine 2.00 (BSF 1167 2008-08-23) MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed Cc: freebsd-hackers@freebsd.org Subject: Re: How to invalidate NFS read cache? X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 12 May 2009 20:56:13 -0000 On Tue, 12 May 2009, Robert Watson wrote: > Normally, NFS clients implement open-to-close consistency, which dictates > that when a close() occurs on client A, all pending writes on the file > should be issued to the server before close() returns, so that a signal to > client B to open() the file can validate its cache before open() returns. This should, of course, read "close-to-open consistency" -- I plead jetlag after an overnight flight back form Boston to the UK :-) Robert N M Watson Computer Laboratory University of Cambridge > > This raises the following question: is client A closing the file, and is > client B then opening it? > > If not: relying on writes being visible on the client B before the close() on > A and a fresh open() on B is not guaranteed to work, although we can discuss > ways to improve behavior with respect to expectation. Try modifying your > application and see if it gets the desired behavior, and then we can discuss > ways to improve what you're seeing. > > If you are: this is probably a bug in our caching and or issuing of NFS RPCs. > We cache both attribute and access data -- perhaps there is an open() path > where we issue neither RPC? In the case of open, we likely should test for a > valid access cache entry, and if there is one, issue an attribute read, and > otherwise just issue an access check which will piggyback fresh attribute > data on the reply. Perhaps there is a bug here somewhere. > > A few other misc questions: > > - Could you confirm you're using NFSv3 on all clients. Are there any special > mount options in use? > - What version of FreeBSD are you running with? > > In FreeBSD 8.x, we now have DTrace probes for all of the above events -- > VOPs, attribute cache hit/miss/load/flush, access cache hit/miss/load/flush, > RPCs, etc, which we can use to debug the problem. I haven't yet MFC'd these > to 7.x, but if you're able to run a very fresh 7-STABLE, I can probably > produce a patch to add it for you in a few days. > > Robert N M Watson > Computer Laboratory > University of Cambridge > From owner-freebsd-hackers@FreeBSD.ORG Tue May 12 21:04:10 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id D7DC51065670 for ; Tue, 12 May 2009 21:04:10 +0000 (UTC) (envelope-from ru@freebsd.org) Received: from mail.vega.ru (mail.vega.ru [90.156.167.5]) by mx1.freebsd.org (Postfix) with ESMTP id 8C6468FC0C for ; Tue, 12 May 2009 21:04:10 +0000 (UTC) (envelope-from ru@freebsd.org) Received: from [10.100.124.99] (port=58922 helo=edoofus.dev.vega.ru) by mail.vega.ru with esmtpsa (TLSv1:AES256-SHA:256) (Exim 4.69 (FreeBSD)) (envelope-from ) id 1M3yef-000Ncc-28; Wed, 13 May 2009 00:32:49 +0400 Date: Wed, 13 May 2009 00:32:44 +0400 From: Ruslan Ermilov To: John Baldwin Message-ID: <20090512203244.GA61891@edoofus.dev.vega.ru> References: <46FDBAFC.1010000@gmail.com> <200905111446.14439.jhb@freebsd.org> <20090511185814.GD1948@deviant.kiev.zoral.com.ua> <200905111623.52881.jhb@freebsd.org> MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <200905111623.52881.jhb@freebsd.org> Cc: Kostik Belousov , freebsd-hackers@freebsd.org, Ighighi Subject: Re: POSIXfy readlink() call X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Tue, 12 May 2009 21:04:11 -0000 On Mon, May 11, 2009 at 04:23:52PM -0400, John Baldwin wrote: > On Monday 11 May 2009 2:58:14 pm Kostik Belousov wrote: > > On Mon, May 11, 2009 at 02:46:14PM -0400, John Baldwin wrote: > > > On Monday 11 May 2009 2:33:09 pm Kostik Belousov wrote: > > > > On Mon, May 11, 2009 at 02:05:07PM -0400, John Baldwin wrote: > > > > > On Friday 28 September 2007 10:39:56 pm Ighighi wrote: > > > > ^^^^^ > > > > > > Yes, I had this stuck in the back of my head from when it first appeared. > > > > > > > > > The POXIX prototype for readlink(2) is: > > > > > > ssize_t readlink(const char *restrict path, char *restrict buf, > size_t > > > > > > bufsize); > > > > > > > > > > It can't simply be corrected as it would change the ABI and thus > requires > > > a > > > > > new system call, etc. However, do you really expect a symlink to be > > > longer > > > > > than 2^31 on a 64-bit machine? > > > > > > > > Yes, I agree that this is ABI change. > > > > > > > > Meantime, > > > > r176215 | ru | 2008-02-12 22:09:04 +0200 (Tue, 12 Feb 2008) | 5 lines > > > > > > > > Change readlink(2)'s return type and type of the last argument > > > > to match POSIX. > > > > > > > > Prodded by: Alexey Lyashkov > > > > > > > > I tried to convince ru@ that ABI breakage is not good, but has not > > > > succeeded. > > > > > > Ugh, is this only in HEAD? If so, I will back it out for 8.0. If this > made > > > it into a release then this is a far bigger mess. Oh, good, this is only > in > > > 8. I will fix this ASAP. I can just add the new syscall I guess. > > > > You need to symver the syscalls. It requires some ugly games with our > > syscall stubs, because gnu ld only honor .symver in the same object where > > the symbol is defined. I did prototyped this some time ago, by including > > a file with appropriate .symver from all stubs. > > So, after thinking about this out loud some more, it seems the ABI breakage > would only be for 64-bit platforms that passed a -ve value as the buffer > size. However, doing so would already either panic due to triggering an > assertion, or result in otherwise undefined behavior and that making the new > parameter unsigned actually results in the same undefined behavior in the > non-panic case. > For the record. I also suggest (re-)reading a thread http://lists.freebsd.org/pipermail/freebsd-current/2008-February/thread.html#83314 that resulted from the original commit where I try to make it clear that a scary ABI breakage Konstantin mentions is pure artificial. Cheers, -- Ruslan Ermilov ru@FreeBSD.org FreeBSD committer From owner-freebsd-hackers@FreeBSD.ORG Wed May 13 23:59:24 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 8319A106564A; Wed, 13 May 2009 23:59:24 +0000 (UTC) (envelope-from des@des.no) Received: from tim.des.no (tim.des.no [194.63.250.121]) by mx1.freebsd.org (Postfix) with ESMTP id 4B27A8FC12; Wed, 13 May 2009 23:59:24 +0000 (UTC) (envelope-from des@des.no) Received: from ds4.des.no (des.no [84.49.246.2]) by smtp.des.no (Postfix) with ESMTP id CB6726D449; Thu, 14 May 2009 01:47:38 +0200 (CEST) Received: by ds4.des.no (Postfix, from userid 1001) id AAEF184497; Thu, 14 May 2009 01:47:38 +0200 (CEST) From: =?utf-8?Q?Dag-Erling_Sm=C3=B8rgrav?= To: alpha@freebsd.org, hackers@freebsd.org Date: Thu, 14 May 2009 01:47:38 +0200 Message-ID: <86tz3o4lb9.fsf@ds4.des.no> User-Agent: Gnus/5.13 (Gnus v5.13) Emacs/23.0.92 (berkeley-unix) MIME-Version: 1.0 Content-Type: text/plain; charset=utf-8 Content-Transfer-Encoding: quoted-printable Cc: Subject: PTE modified bit emulation trap X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Wed, 13 May 2009 23:59:24 -0000 Coverity complains about the lack of error checking in the following code in sys/kern/kern_sysctl.c, around line 1390: /* * Touch all the wired pages to avoid PTE modified * bit emulation traps on Alpha while holding locks * in the sysctl handler. */ for (i =3D (wiredlen + PAGE_SIZE - 1) / PAGE_SIZE, cp =3D req->oldptr; i > 0; i--, cp +=3D PAGE_SIZE) { copyin(cp, &dummy, 1); copyout(&dummy, cp, 1); } Since Alpha is dead, can we remove this, or is it still needed for other platforms? DES --=20 Dag-Erling Sm=C3=B8rgrav - des@des.no From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 03:25:09 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 53EA61065670 for ; Thu, 14 May 2009 03:25:09 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: from gdead.mooseriver.com (gdead.mooseriver.com [205.166.121.45]) by mx1.freebsd.org (Postfix) with ESMTP id 330478FC08; Thu, 14 May 2009 03:25:09 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: by gdead.mooseriver.com (Postfix, from userid 2010) id 52E0C63389; Wed, 13 May 2009 20:06:36 -0700 (PDT) X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gdead.mooseriver.com X-Spam-Level: X-Spam-Status: No, score=-2.7 required=5.0 tests=AWL,BAYES_00 autolearn=ham version=3.2.5 Received: from mooseriver.com (berkeley.mooseriver.com [75.61.201.134]) by gdead.mooseriver.com (Postfix) with ESMTP id A89C76336A; Wed, 13 May 2009 20:06:34 -0700 (PDT) Received: from berkeley.mooseriver.com (localhost [127.0.0.1]) by mooseriver.com (Postfix) with ESMTP id 7A0F318141B; Wed, 13 May 2009 20:06:34 -0700 (PDT) Received: (from jgrosch@localhost) by berkeley.mooseriver.com (8.14.3/8.14.3/Submit) id n4E36YM3001377; Wed, 13 May 2009 20:06:34 -0700 (PDT) (envelope-from jgrosch@mooseriver.com) X-Authentication-Warning: berkeley.mooseriver.com: jgrosch set sender to jgrosch@mooseriver.com using -f Date: Wed, 13 May 2009 20:06:34 -0700 From: Josef Grosch To: hackers@freebsd.org Message-ID: <20090514030634.GA1252@mooseriver.com> Mime-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="x+6KMIRAuhnl3hBn" Content-Disposition: inline User-Agent: Mutt/1.4.2.3i Organization: Moose River, LLC Cc: question@freebsd.org Subject: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: jgrosch@mooseriver.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 03:25:09 -0000 --x+6KMIRAuhnl3hBn Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable I'm in search for a decent video card. I currently have an Nvidia GeForce 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home machine and I am running amd64 FreeBSD 7.2 and it just refuses to go into X. It just hangs. I've been poking around and, based on what I read, some FreeBSD developers and Nvidia have gotten into a finger pointing contest as to what is the problem. Its all very nice but doesn't help me much. So, can any one recommend a good video card? What I'm looking for is * Works with amd64 FreeBSD 7.2 * DVI=20 * PCI-E x16 * 512 MB or more * Not going to cost an arm and a leg Thanks Josef --=20 Josef Grosch | Another day closer to a | FreeBSD 7.2 jgrosch@MooseRiver.com | Micro$oft free world | Berkeley, Ca. --x+6KMIRAuhnl3hBn Content-Type: application/pgp-signature Content-Disposition: inline -----BEGIN PGP SIGNATURE----- iD8DBQFKC4q6y8prLS1GYSERAtxcAJ9IFDAhVN10Ht1oNsh+sSUo+TRn2wCdGjba LvLiQUIUtDIPU8BvukeNMr0= =q8nO -----END PGP SIGNATURE----- --x+6KMIRAuhnl3hBn-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 04:06:06 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 5A46D106566B for ; Thu, 14 May 2009 04:06:06 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: from gdead.mooseriver.com (gdead.mooseriver.com [205.166.121.45]) by mx1.freebsd.org (Postfix) with ESMTP id 35DA58FC12; Thu, 14 May 2009 04:06:06 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: by gdead.mooseriver.com (Postfix, from userid 2010) id 1C98A6333C; Wed, 13 May 2009 21:06:06 -0700 (PDT) X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gdead.mooseriver.com X-Spam-Level: X-Spam-Status: No, score=-2.7 required=5.0 tests=AWL,BAYES_00 autolearn=ham version=3.2.5 Received: from mooseriver.com (berkeley.mooseriver.com [75.61.201.134]) by gdead.mooseriver.com (Postfix) with ESMTP id 8CF3463338; Wed, 13 May 2009 21:06:04 -0700 (PDT) Received: from berkeley.mooseriver.com (localhost [127.0.0.1]) by mooseriver.com (Postfix) with ESMTP id 667AB18141B; Wed, 13 May 2009 21:06:04 -0700 (PDT) Received: (from jgrosch@localhost) by berkeley.mooseriver.com (8.14.3/8.14.3/Submit) id n4E4642i001757; Wed, 13 May 2009 21:06:04 -0700 (PDT) (envelope-from jgrosch@mooseriver.com) X-Authentication-Warning: berkeley.mooseriver.com: jgrosch set sender to jgrosch@mooseriver.com using -f Date: Wed, 13 May 2009 21:06:04 -0700 From: Josef Grosch To: "Sam Fourman Jr." Message-ID: <20090514040604.GA1418@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> <11167f520905132045j57fc8914n40894ceecbf33ee5@mail.gmail.com> Mime-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="PNTmBPCT7hxwcZjr" Content-Disposition: inline In-Reply-To: <11167f520905132045j57fc8914n40894ceecbf33ee5@mail.gmail.com> User-Agent: Mutt/1.4.2.3i Organization: Moose River, LLC Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: jgrosch@mooseriver.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 04:06:06 -0000 --PNTmBPCT7hxwcZjr Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable On Wed, May 13, 2009 at 10:45:17PM -0500, Sam Fourman Jr. wrote: > On Wed, May 13, 2009 at 10:06 PM, Josef Grosch w= rote: > > > > I'm in search for a decent video card. I currently have an Nvidia GeFor= ce > > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go in= to > > X. It just hangs. I've been poking around and, based on what I read, so= me > > FreeBSD developers and Nvidia have gotten into a finger pointing contes= t as > > to what is the problem. Its all very nice but doesn't help me much. >=20 > I can shed some light on the amd64 binary nvidia driver issue > John Baldwin has implimented the features the Nvidia people need. >=20 > http://www.freebsd.org/news/status/report-2009-01-2009-03.html#Device-mma= p()-Extensions >=20 > if you read the nvnews fourms Zander made refrence to working on a 64bit = driver. >=20 >=20 > Sam Fourman Jr. Great! So there is hope for my Nvidia card.=20 Josef --=20 Josef Grosch | Another day closer to a | FreeBSD 7.2 jgrosch@MooseRiver.com | Micro$oft free world | Berkeley, Ca. --PNTmBPCT7hxwcZjr Content-Type: application/pgp-signature Content-Disposition: inline -----BEGIN PGP SIGNATURE----- iD8DBQFKC5isy8prLS1GYSERAlnmAJ9tJHzybHRYCHLl1R+ZkXQsFjJ6yQCeM6K4 P4qr0zf38ydQFL3JTX2KOwA= =Iw6Q -----END PGP SIGNATURE----- --PNTmBPCT7hxwcZjr-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 04:10:16 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id E12A01065673 for ; Thu, 14 May 2009 04:10:16 +0000 (UTC) (envelope-from sfourman@gmail.com) Received: from mail-qy0-f173.google.com (mail-qy0-f173.google.com [209.85.221.173]) by mx1.freebsd.org (Postfix) with ESMTP id 836508FC19; Thu, 14 May 2009 04:10:16 +0000 (UTC) (envelope-from sfourman@gmail.com) Received: by qyk3 with SMTP id 3so2056946qyk.3 for ; Wed, 13 May 2009 21:10:11 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type :content-transfer-encoding; bh=wIy6bwN1+03+BQ9Ixb0wphBs1n3FkfXyZkpfxCPNxJk=; b=PbQoiXOjiU+HIhl43+c4xBqx3lmxjojlPdtI8MG+yEMHI0X3CjgGw8SeCkWXEOC9R1 GBY2lHTAwfxCtP5Y2xSV1nGfnFHPgoszDtGEv8g81Tl05CGXMwD7KnXiU0WIiRvIlvm4 ONdhlyRjuAytKNR4ix8odJAL2cRKOdwvDGWMQ= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type:content-transfer-encoding; b=a8vcvtvJhmL4eeRe37M7uZ1vEGR/qdwgkSQpsFA/NgloEt1GswPWU9Z9z9WYUfBraM HThLhFwJFxSmXTlxQTHez1zsb8wTBd5Fyy9tl8ce29UkToxHZbeYd5/ZI7GW7vtIw67n 1UpuUwruLjau7s95HPjplTKqx/eGeXvZyz9JA= MIME-Version: 1.0 Received: by 10.229.110.5 with SMTP id l5mr1400778qcp.88.1242272717062; Wed, 13 May 2009 20:45:17 -0700 (PDT) In-Reply-To: <20090514030634.GA1252@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> Date: Wed, 13 May 2009 22:45:17 -0500 Message-ID: <11167f520905132045j57fc8914n40894ceecbf33ee5@mail.gmail.com> From: "Sam Fourman Jr." To: jgrosch@mooseriver.com Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 04:10:17 -0000 On Wed, May 13, 2009 at 10:06 PM, Josef Grosch wrote: > > I'm in search for a decent video card. I currently have an Nvidia GeForce > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go into > X. It just hangs. I've been poking around and, based on what I read, some > FreeBSD developers and Nvidia have gotten into a finger pointing contest as > to what is the problem. Its all very nice but doesn't help me much. I can shed some light on the amd64 binary nvidia driver issue John Baldwin has implimented the features the Nvidia people need. http://www.freebsd.org/news/status/report-2009-01-2009-03.html#Device-mmap()-Extensions if you read the nvnews fourms Zander made refrence to working on a 64bit driver. Sam Fourman Jr. From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 04:18:36 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 9F288106566C for ; Thu, 14 May 2009 04:18:36 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: from gdead.mooseriver.com (gdead.mooseriver.com [205.166.121.45]) by mx1.freebsd.org (Postfix) with ESMTP id 7B72E8FC1E; Thu, 14 May 2009 04:18:36 +0000 (UTC) (envelope-from jgrosch@mooseriver.com) Received: by gdead.mooseriver.com (Postfix, from userid 2010) id 5E63D63347; Wed, 13 May 2009 21:18:36 -0700 (PDT) X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gdead.mooseriver.com X-Spam-Level: X-Spam-Status: No, score=-2.8 required=5.0 tests=AWL,BAYES_00 autolearn=ham version=3.2.5 Received: from mooseriver.com (berkeley.mooseriver.com [75.61.201.134]) by gdead.mooseriver.com (Postfix) with ESMTP id 635896333C; Wed, 13 May 2009 21:18:34 -0700 (PDT) Received: from berkeley.mooseriver.com (localhost [127.0.0.1]) by mooseriver.com (Postfix) with ESMTP id 3DF5A18141B; Wed, 13 May 2009 21:18:34 -0700 (PDT) Received: (from jgrosch@localhost) by berkeley.mooseriver.com (8.14.3/8.14.3/Submit) id n4E4IYmn001829; Wed, 13 May 2009 21:18:34 -0700 (PDT) (envelope-from jgrosch@mooseriver.com) X-Authentication-Warning: berkeley.mooseriver.com: jgrosch set sender to jgrosch@mooseriver.com using -f Date: Wed, 13 May 2009 21:18:34 -0700 From: Josef Grosch To: Mike Meyer Message-ID: <20090514041834.GB1418@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> <20090514000203.3d053800@bhuda.mired.org> Mime-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="kORqDWCi7qDJ0mEj" Content-Disposition: inline In-Reply-To: <20090514000203.3d053800@bhuda.mired.org> User-Agent: Mutt/1.4.2.3i Organization: Moose River, LLC Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: jgrosch@mooseriver.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 04:18:36 -0000 --kORqDWCi7qDJ0mEj Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable On Thu, May 14, 2009 at 12:02:03AM -0400, Mike Meyer wrote: > On Wed, 13 May 2009 20:06:34 -0700 > Josef Grosch wrote: >=20 > >=20 > > I'm in search for a decent video card. I currently have an Nvidia GeFor= ce > > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go in= to > > X. It just hangs. I've been poking around and, based on what I read, so= me > > FreeBSD developers and Nvidia have gotten into a finger pointing contes= t as > > to what is the problem. Its all very nice but doesn't help me much. > >=20 > > So, can any one recommend a good video card? What I'm looking for is > >=20 > > * Works with amd64 FreeBSD 7.2 > > * DVI=20 > > * PCI-E x16 > > * 512 MB or more > > * Not going to cost an arm and a leg >=20 > You forgot the critical information: you didn't define what works for > you. In particular, does a card that doesn't do 3d acceleration > "work"? How about 2d? >=20 > The open source Nvidia driver pretty much sucks. Probably because the > proprietary Nvidia blob (which you were presumably using on i386) is > one of the most functional X video drivers around, so there's not a > lot of incentive to work on the open source version. But you can't use > the proprietary blob on amd64, so you get the open source driver, and > - well you've experienced it. >=20 > The ATI radeon driver - it's open source, there's no proprietary blob > - is actually pretty good. Except that 2d & 3d acceleration support > is, um, variable. >=20 > If you have to have 2d & 3d acceleration, I don't believe you have a > good option for FreeBSD on amd64, at least not until the kernel tweaks > Nvidia needs are done (there has been some motion on that front > recently). But I don't really need it, so I haven't spent any time > looking for such a card. >=20 > If you're ok with solid - if basic - video performance, I'll recommend > pretty much any radeon card. I've used a number of them to drive dual > 1920x1200 displays on a variety of systems for a couple of years now. > Amazon has cards that meet your listed requirements for under US$40. >=20 > Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id BB1F2106566C for ; Thu, 14 May 2009 04:30:17 +0000 (UTC) (envelope-from mwm-keyword-freebsdhackers2.e313df@mired.org) Received: from mired.org (two.mired.org [74.143.213.43]) by mx1.freebsd.org (Postfix) with ESMTP id 776C48FC0A for ; Thu, 14 May 2009 04:30:17 +0000 (UTC) (envelope-from mwm-keyword-freebsdhackers2.e313df@mired.org) Received: (qmail 29538 invoked by uid 1001); 14 May 2009 00:02:04 -0400 Received: from bhuda.mired.org (localhost.localdomain [127.0.0.1]) by bhuda (tmda-ofmipd) with ESMTP; Thu, 14 May 2009 00:02:03 -0400 Date: Thu, 14 May 2009 00:02:03 -0400 To: jgrosch@mooseriver.com Message-ID: <20090514000203.3d053800@bhuda.mired.org> In-Reply-To: <20090514030634.GA1252@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> Organization: Meyer Consulting X-Mailer: Claws Mail 3.7.1 (GTK+ 2.14.7; amd64-portbld-freebsd7.1) Face: iVBORw0KGgoAAAANSUhEUgAAADAAAAAwBAMAAAClLOS0AAAAG1BMVEXguIzRkGnhyaz069mXhW0WHRnbrnR9WCQ6LB0CchNMAAACSUlEQVQ4jV2TQW7jMAxFGaPQOgQEdZaGMsgBrAvUA03dCxj1Uu4U2gfwQD7AGNax51NK07RcxXz6/CSl0Ij450vkPG1jzpIZM1UwDCl/xB14TWnNX8A00Qj5a0mnVFVbVUz4MeErea2HikSRqZzY894zwg9p2+/AtO8LzxFED+tNAUFeU29iFOLRxlZAcdo9A8wi8ZBMV4BKPde82Oxrvs6BTkulQIClte0DLFzzsKk9j1MBex8iUaP00Bd78S/muyFScrTXz6zLkEUxJp+SabQfNOs4f4Jpx5qSZ/304PWwlEWP1cOn/mJQR7EOD+uKhjcBLziuL7xoY5Xm+VFAUSw/LwwwsHEHxihpwV4EJH0xXRkbw1PkRw+X4pEuSJwBggqk+HEYKkiL5/74/nQkogigzQsAFrakxZyfw3wMIEEZPv4AWMfxwqE5GNxGaERjmH+PG8AE0L4/w9g0lsp1raLYAN5azQa+AOoO9NwcpFkTrG2VKNMNEL5UKUUAw34tha0z7onUG0oBoNtczE04GwFE3wCHc0ChezAJ6A1WMV81AtY7wDAJSlXwV+4cwBvsOsrQMRawfQEBz0deEZ7WNpV2szckIKo5VpDHDSDvF1GItwqqAlG01Hh50BGtVhuUkjkasg/14bYFGCgWg1fSWHvmOoJck2xdp9ZvZBHzDVTzX23TkrOn7qe5U2COEw5D4Vx3qEQpFY2Z/3QFnJxzp7YCmSMG19nOUoe869zZfOQb5ywQuWu0yCn5+8gxZz+BE7vG3j4/wbf4D/sXN9Wug1s7AAAAAElFTkSuQmCC Mime-Version: 1.0 Content-Type: text/plain; charset=US-ASCII Content-Transfer-Encoding: 7bit X-Delivery-Agent: TMDA/1.1.12 (Macallan) From: Mike Meyer Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 04:30:18 -0000 On Wed, 13 May 2009 20:06:34 -0700 Josef Grosch wrote: > > I'm in search for a decent video card. I currently have an Nvidia GeForce > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go into > X. It just hangs. I've been poking around and, based on what I read, some > FreeBSD developers and Nvidia have gotten into a finger pointing contest as > to what is the problem. Its all very nice but doesn't help me much. > > So, can any one recommend a good video card? What I'm looking for is > > * Works with amd64 FreeBSD 7.2 > * DVI > * PCI-E x16 > * 512 MB or more > * Not going to cost an arm and a leg You forgot the critical information: you didn't define what works for you. In particular, does a card that doesn't do 3d acceleration "work"? How about 2d? The open source Nvidia driver pretty much sucks. Probably because the proprietary Nvidia blob (which you were presumably using on i386) is one of the most functional X video drivers around, so there's not a lot of incentive to work on the open source version. But you can't use the proprietary blob on amd64, so you get the open source driver, and - well you've experienced it. The ATI radeon driver - it's open source, there's no proprietary blob - is actually pretty good. Except that 2d & 3d acceleration support is, um, variable. If you have to have 2d & 3d acceleration, I don't believe you have a good option for FreeBSD on amd64, at least not until the kernel tweaks Nvidia needs are done (there has been some motion on that front recently). But I don't really need it, so I haven't spent any time looking for such a card. If you're ok with solid - if basic - video performance, I'll recommend pretty much any radeon card. I've used a number of them to drive dual 1920x1200 displays on a variety of systems for a couple of years now. Amazon has cards that meet your listed requirements for under US$40. http://www.mired.org/consulting.html Independent Network/Unix/Perforce consultant, email for more information. O< ascii ribbon campaign - stop html mail - www.asciiribbon.org From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 06:10:37 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 56A5D1065675 for ; Thu, 14 May 2009 06:10:37 +0000 (UTC) (envelope-from adrian.chadd@gmail.com) Received: from mail-qy0-f173.google.com (mail-qy0-f173.google.com [209.85.221.173]) by mx1.freebsd.org (Postfix) with ESMTP id EA5638FC0A; Thu, 14 May 2009 06:10:36 +0000 (UTC) (envelope-from adrian.chadd@gmail.com) Received: by qyk3 with SMTP id 3so2136002qyk.3 for ; Wed, 13 May 2009 23:10:36 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:sender:received:in-reply-to :references:date:x-google-sender-auth:message-id:subject:from:to:cc :content-type:content-transfer-encoding; bh=hFOdcxt+VwWNC1dxaDkS0Kf0pnVnj+ql1kSYHpdTsO8=; b=EBamkHhSVPQPc64SbiPxnxTX0jIG6VWl4tZVHY7Ajg4CV9sa7nUGjpCG3iULAhaPxJ /6+x/i9SMen4xkO4KF/lqmiFV1fW/7cQGE3a21yVb0Oy7feZIAQ4iSamyp+1bDgh1KJT +/Fe/f+VVj0TvdVbdvZoO8bIRTVBXPUb7TqAw= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:sender:in-reply-to:references:date :x-google-sender-auth:message-id:subject:from:to:cc:content-type :content-transfer-encoding; b=pbTqj1EZVlEojdALGTaQYEHzdr4ngGL0ISgjJNnQwYYCNJPp66C+3W4InVTp/1Y/DM Vc1LovztwlMq3wgCSknB6Yy+WxvskNI4KGE3sh6YrUrxhJYA/NvmthLP2Pj5+4gy3BHF QVYLy1cXa0hUZT+MAjJctCUJ9zs7xvcTCb3OA= MIME-Version: 1.0 Sender: adrian.chadd@gmail.com Received: by 10.229.97.19 with SMTP id j19mr1458822qcn.54.1242279740425; Wed, 13 May 2009 22:42:20 -0700 (PDT) In-Reply-To: <20090514041834.GB1418@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> <20090514000203.3d053800@bhuda.mired.org> <20090514041834.GB1418@mooseriver.com> Date: Thu, 14 May 2009 13:42:20 +0800 X-Google-Sender-Auth: 8642bb55c9fa96f8 Message-ID: From: Adrian Chadd To: jgrosch@mooseriver.com Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit Cc: hackers@freebsd.org, question@freebsd.org, Mike Meyer Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 06:10:37 -0000 2009/5/14 Josef Grosch : > I don't need 2d & 3d acceleration. I just need a card that will handle > WindowMaker on a 24 inch Dell monitor at 1920x1200 and as long as the flesh > tones on my JPGs don't suck I'm happy. > > Thanks for the advice. I guess I'm going to make a trip to Fry's Friday. I've experienced no-acceleration radeon driver "desktop" under Ubuntu and FreeBSD; let me please point out how sluggish and horribly slow it is. I gave up trying to get accelerated 3d + dualhead support on the card(s) I was using - apparently the hardware just didn't do a single viewport span across 2 1280x1024 screens :( (The max viewport width was 2048 pixels..) 2d acceleration may be a must for that kind of resolution.. YMMV (and obviously, please report back your findings!) adrian From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 07:08:02 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id EDE00106566C; Thu, 14 May 2009 07:08:02 +0000 (UTC) (envelope-from doconnor@gsoft.com.au) Received: from cain.gsoft.com.au (cain.gsoft.com.au [203.31.81.10]) by mx1.freebsd.org (Postfix) with ESMTP id 403DB8FC12; Thu, 14 May 2009 07:08:01 +0000 (UTC) (envelope-from doconnor@gsoft.com.au) Received: from inchoate.gsoft.com.au (inchoate.gsoft.com.au [203.31.81.30]) (authenticated bits=0) by cain.gsoft.com.au (8.13.8/8.13.8) with ESMTP id n4E6eH9n098289 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES128-SHA bits=128 verify=NO); Thu, 14 May 2009 16:10:17 +0930 (CST) (envelope-from doconnor@gsoft.com.au) From: "Daniel O'Connor" To: freebsd-hackers@freebsd.org Date: Thu, 14 May 2009 16:10:07 +0930 User-Agent: KMail/1.9.10 References: <20090514030634.GA1252@mooseriver.com> <20090514041834.GB1418@mooseriver.com> In-Reply-To: MIME-Version: 1.0 Content-Type: multipart/signed; boundary="nextPart1318273.vxGJtxcTYF"; protocol="application/pgp-signature"; micalg=pgp-sha1 Content-Transfer-Encoding: 7bit Message-Id: <200905141610.15344.doconnor@gsoft.com.au> X-Spam-Score: -3.499 () ALL_TRUSTED,AWL,BAYES_00 X-Scanned-By: MIMEDefang 2.63 on 203.31.81.10 Cc: question@freebsd.org, Adrian Chadd , hackers@freebsd.org, Mike Meyer Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 07:08:03 -0000 --nextPart1318273.vxGJtxcTYF Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: quoted-printable Content-Disposition: inline On Thu, 14 May 2009, Adrian Chadd wrote: > 2009/5/14 Josef Grosch : > > I don't need 2d & 3d acceleration. I just need a card that will > > handle WindowMaker on a 24 inch Dell monitor at 1920x1200 and as > > long as the flesh tones on my JPGs don't suck I'm happy. > > > > Thanks for the advice. I guess I'm going to make a trip to Fry's > > Friday. > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > and FreeBSD; let me please point out how sluggish and horribly slow > it is. Depends how unaccelerated it is. VESA is pretty damn slow, but even minimal radeon/radeonhd support is=20 fast enough for desktop use. > I gave up trying to get accelerated 3d + dualhead support on the > card(s) I was using - apparently the hardware just didn't do a single > viewport span across 2 1280x1024 screens :( > (The max viewport width was 2048 pixels..) > > 2d acceleration may be a must for that kind of resolution.. If you have a fast CPU & decent pipe to video memory it isn't necessary,=20 but very nice. =2D-=20 Daniel O'Connor software and network engineer for Genesis Software - http://www.gsoft.com.au "The nice thing about standards is that there are so many of them to choose from." -- Andrew Tanenbaum GPG Fingerprint - 5596 B766 97C0 0E94 4347 295E E593 DC20 7B3F CE8C --nextPart1318273.vxGJtxcTYF Content-Type: application/pgp-signature; name=signature.asc Content-Description: This is a digitally signed message part. -----BEGIN PGP SIGNATURE----- Version: GnuPG v2.0.11 (FreeBSD) iD8DBQBKC7zP5ZPcIHs/zowRAoaFAKCCtdj55kz4pmZ8V3Oyrilpi9WyaQCfU9jx 8UWur6KSfXfIpb5WCIeyD1c= =tout -----END PGP SIGNATURE----- --nextPart1318273.vxGJtxcTYF-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 07:08:02 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id EDE00106566C; Thu, 14 May 2009 07:08:02 +0000 (UTC) (envelope-from doconnor@gsoft.com.au) Received: from cain.gsoft.com.au (cain.gsoft.com.au [203.31.81.10]) by mx1.freebsd.org (Postfix) with ESMTP id 403DB8FC12; Thu, 14 May 2009 07:08:01 +0000 (UTC) (envelope-from doconnor@gsoft.com.au) Received: from inchoate.gsoft.com.au (inchoate.gsoft.com.au [203.31.81.30]) (authenticated bits=0) by cain.gsoft.com.au (8.13.8/8.13.8) with ESMTP id n4E6eH9n098289 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES128-SHA bits=128 verify=NO); Thu, 14 May 2009 16:10:17 +0930 (CST) (envelope-from doconnor@gsoft.com.au) From: "Daniel O'Connor" To: freebsd-hackers@freebsd.org Date: Thu, 14 May 2009 16:10:07 +0930 User-Agent: KMail/1.9.10 References: <20090514030634.GA1252@mooseriver.com> <20090514041834.GB1418@mooseriver.com> In-Reply-To: MIME-Version: 1.0 Content-Type: multipart/signed; boundary="nextPart1318273.vxGJtxcTYF"; protocol="application/pgp-signature"; micalg=pgp-sha1 Content-Transfer-Encoding: 7bit Message-Id: <200905141610.15344.doconnor@gsoft.com.au> X-Spam-Score: -3.499 () ALL_TRUSTED,AWL,BAYES_00 X-Scanned-By: MIMEDefang 2.63 on 203.31.81.10 Cc: question@freebsd.org, Adrian Chadd , hackers@freebsd.org, Mike Meyer Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 07:08:03 -0000 --nextPart1318273.vxGJtxcTYF Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: quoted-printable Content-Disposition: inline On Thu, 14 May 2009, Adrian Chadd wrote: > 2009/5/14 Josef Grosch : > > I don't need 2d & 3d acceleration. I just need a card that will > > handle WindowMaker on a 24 inch Dell monitor at 1920x1200 and as > > long as the flesh tones on my JPGs don't suck I'm happy. > > > > Thanks for the advice. I guess I'm going to make a trip to Fry's > > Friday. > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > and FreeBSD; let me please point out how sluggish and horribly slow > it is. Depends how unaccelerated it is. VESA is pretty damn slow, but even minimal radeon/radeonhd support is=20 fast enough for desktop use. > I gave up trying to get accelerated 3d + dualhead support on the > card(s) I was using - apparently the hardware just didn't do a single > viewport span across 2 1280x1024 screens :( > (The max viewport width was 2048 pixels..) > > 2d acceleration may be a must for that kind of resolution.. If you have a fast CPU & decent pipe to video memory it isn't necessary,=20 but very nice. =2D-=20 Daniel O'Connor software and network engineer for Genesis Software - http://www.gsoft.com.au "The nice thing about standards is that there are so many of them to choose from." -- Andrew Tanenbaum GPG Fingerprint - 5596 B766 97C0 0E94 4347 295E E593 DC20 7B3F CE8C --nextPart1318273.vxGJtxcTYF Content-Type: application/pgp-signature; name=signature.asc Content-Description: This is a digitally signed message part. -----BEGIN PGP SIGNATURE----- Version: GnuPG v2.0.11 (FreeBSD) iD8DBQBKC7zP5ZPcIHs/zowRAoaFAKCCtdj55kz4pmZ8V3Oyrilpi9WyaQCfU9jx 8UWur6KSfXfIpb5WCIeyD1c= =tout -----END PGP SIGNATURE----- --nextPart1318273.vxGJtxcTYF-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 09:13:22 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 70CED1065674 for ; Thu, 14 May 2009 09:13:22 +0000 (UTC) (envelope-from rdivacky@vlk.vlakno.cz) Received: from vlakno.cz (77-93-215-190.static.masterinter.net [77.93.215.190]) by mx1.freebsd.org (Postfix) with ESMTP id 25F808FC08 for ; Thu, 14 May 2009 09:13:21 +0000 (UTC) (envelope-from rdivacky@vlk.vlakno.cz) Received: from localhost (localhost [127.0.0.1]) by vlakno.cz (Postfix) with ESMTP id 08EE19CB0F7; Thu, 14 May 2009 11:12:55 +0200 (CEST) X-Virus-Scanned: amavisd-new at vlakno.cz Received: from vlakno.cz ([127.0.0.1]) by localhost (lev.vlakno.cz [127.0.0.1]) (amavisd-new, port 10024) with ESMTP id 3f8CnrVdmbW1; Thu, 14 May 2009 11:12:52 +0200 (CEST) Received: from vlk.vlakno.cz (localhost [127.0.0.1]) by vlakno.cz (Postfix) with ESMTP id C0B759CB110; Thu, 14 May 2009 11:12:52 +0200 (CEST) Received: (from rdivacky@localhost) by vlk.vlakno.cz (8.14.3/8.14.3/Submit) id n4E9Cqgk004523; Thu, 14 May 2009 11:12:52 +0200 (CEST) (envelope-from rdivacky) Date: Thu, 14 May 2009 11:12:52 +0200 From: Roman Divacky To: Josef Grosch Message-ID: <20090514091252.GA4341@freebsd.org> References: <20090514030634.GA1252@mooseriver.com> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <20090514030634.GA1252@mooseriver.com> User-Agent: Mutt/1.4.2.3i Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 09:13:22 -0000 On Wed, May 13, 2009 at 08:06:34PM -0700, Josef Grosch wrote: > > I'm in search for a decent video card. I currently have an Nvidia GeForce > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go into > X. It just hangs. I've been poking around and, based on what I read, some > FreeBSD developers and Nvidia have gotten into a finger pointing contest as > to what is the problem. Its all very nice but doesn't help me much. > > So, can any one recommend a good video card? What I'm looking for is > > * Works with amd64 FreeBSD 7.2 > * DVI > * PCI-E x16 > * 512 MB or more > * Not going to cost an arm and a leg you can try nouveau driver in the meantime From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 09:57:56 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id D7EBC1065678 for ; Thu, 14 May 2009 09:57:56 +0000 (UTC) (envelope-from xorquewasp@googlemail.com) Received: from mail-ew0-f159.google.com (mail-ew0-f159.google.com [209.85.219.159]) by mx1.freebsd.org (Postfix) with ESMTP id 655068FC24 for ; Thu, 14 May 2009 09:57:56 +0000 (UTC) (envelope-from xorquewasp@googlemail.com) Received: by ewy3 with SMTP id 3so1391030ewy.43 for ; Thu, 14 May 2009 02:57:55 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=googlemail.com; s=gamma; h=domainkey-signature:received:received:received:date:from:to:cc :subject:message-id:references:mime-version:content-type :content-disposition:in-reply-to; bh=l9zlXYZ60BsCwhi0fxYCoAzsusyN6oi3DFB44Gi7qFw=; b=meu7kuyVOXZoVyCWw09sPWpYik5KMfg14mY/CQjFlOXtv7zLc3vilYVlvVOgziAhRN 24JkyRQ+pj7tGiQ6PoZyVkoHve9B7rLlmLeznuJGfqrWPeOk3q5d31gE15JeGkOdarCa G8Ps+NH4N0DG2C/9ZoOZpLMN6npW5KedxAcmU= DomainKey-Signature: a=rsa-sha1; c=nofws; d=googlemail.com; s=gamma; h=date:from:to:cc:subject:message-id:references:mime-version :content-type:content-disposition:in-reply-to; b=hQbRkxTkOf5Oxmf/CF7kLhvsgCS5rbjn+7oeVYlOwjhFrxU4CgAt+IUNZpMoImcRzA fwIH6DipkqAiomyVe9MvwnRs/3Xqfv2wxyhrPn3RtQwtWZxdoT/DukQAd3hHMZzQcbAl TpEZuDHuu5WQLw31GHvWCEk/4KqshJWvptecw= Received: by 10.210.37.11 with SMTP id k11mr2512476ebk.9.1242293384117; Thu, 14 May 2009 02:29:44 -0700 (PDT) Received: from logik.internal.network (81-86-41-187.dsl.pipex.com [81.86.41.187]) by mx.google.com with ESMTPS id 8sm1180181ewy.37.2009.05.14.02.29.43 (version=TLSv1/SSLv3 cipher=OTHER); Thu, 14 May 2009 02:29:43 -0700 (PDT) Received: by logik.internal.network (Postfix, from userid 11001) id 8C2215C31; Thu, 14 May 2009 09:29:38 +0000 (UTC) Date: Thu, 14 May 2009 10:29:38 +0100 From: xorquewasp@googlemail.com To: Josef Grosch Message-ID: <20090514092938.GA14415@logik.internal.network> References: <20090514030634.GA1252@mooseriver.com> MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <20090514030634.GA1252@mooseriver.com> Cc: hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 09:57:57 -0000 On 2009-05-13 20:06:34, Josef Grosch wrote: > I'm in search for a decent video card. I had to do the same thing recently. I wanted dual head (2x 1440x800), 3D accelerated, PCI Express, AMD64 capable graphics. Finally settled on a Radeon x1950, specifically the Powercolor x1950. The prices vary wildly, I got mine off ebay for about $80 but I've seen people attempt to charge ~$200. Don't let someone rip you off... So far, the card's been absolutely stable. I have a dual-head setup with two identical monitors and the card gives excellent performance for OpenGL work. Running FreeBSD 7.2-RELEASE-amd64. xw From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 11:35:38 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 63A99106566C for ; Thu, 14 May 2009 11:35:38 +0000 (UTC) (envelope-from screwdriver@lxnt.info) Received: from mail.lxnt.info (mail.lxnt.info [94.124.200.23]) by mx1.freebsd.org (Postfix) with ESMTP id 2199F8FC26 for ; Thu, 14 May 2009 11:35:38 +0000 (UTC) (envelope-from screwdriver@lxnt.info) Received: from [94.124.202.131] (helo=[192.168.3.144]) by mail.lxnt.info with esmtpa (Exim 4.69 (FreeBSD)) (envelope-from ) id 1M4Yt5-000EtA-7T; Thu, 14 May 2009 15:14:07 +0400 Message-ID: <4A0BFCFE.2070907@lxnt.info> Date: Thu, 14 May 2009 15:14:06 +0400 From: Alexander Sabourenkov User-Agent: Thunderbird 2.0.0.21 (X11/20090318) MIME-Version: 1.0 To: Josef Grosch References: <20090514030634.GA1252@mooseriver.com> <20090514092938.GA14415@logik.internal.network> In-Reply-To: <20090514092938.GA14415@logik.internal.network> Content-Type: text/plain; charset=ISO-8859-1; format=flowed Content-Transfer-Encoding: 7bit Cc: hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 11:35:38 -0000 xorquewasp@googlemail.com wrote: > Finally settled on a Radeon x1950 I second that. PCIe X1950Pro with 256Mb RAM is best card price/{performance, stability} - wise you can get right now. -- ./lxnt From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 11:44:00 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id ED8A51065670 for ; Thu, 14 May 2009 11:44:00 +0000 (UTC) (envelope-from o.petrachev@sprinthost.ru) Received: from odin.from.sh (odin.from.sh [80.93.50.112]) by mx1.freebsd.org (Postfix) with ESMTP id AA03C8FC15 for ; Thu, 14 May 2009 11:44:00 +0000 (UTC) (envelope-from o.petrachev@sprinthost.ru) Received: from [89.223.116.161] (helo=[10.10.10.126]) by odin.from.sh with esmtpa (Exim 4.69 (FreeBSD)) (envelope-from ) id 1M4ZBv-000PMB-Ee for freebsd-hackers@freebsd.org; Thu, 14 May 2009 15:33:35 +0400 Message-ID: <4A0C0187.1030107@sprinthost.ru> Date: Thu, 14 May 2009 15:33:27 +0400 From: =?UTF-8?B?0J7Qu9C10LMg0J/QtdGC0YDQsNGH0ZHQsg==?= User-Agent: Thunderbird 2.0.0.21 (X11/20090318) MIME-Version: 1.0 To: freebsd-hackers@freebsd.org Content-Type: text/plain; charset=UTF-8; format=flowed Content-Transfer-Encoding: 7bit X-Mailman-Approved-At: Thu, 14 May 2009 11:49:39 +0000 Subject: ipfw uid rules for lo0 interface X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 11:44:01 -0000 Hello! I am using FreeBSD 7.2-RELEASE. I am trying to restrict connections to local smtp daemon to limited number of users. But when I create rules for ipfw with uid pattern, I don't get the desired result: all connections on 25 port are blocked and it is impossible to allow it for anyone. I am using the following rules (let's say only root is allowed send messages): # ipfw flush # ipfw add 100 allow ip from any to me 25 uid root # ipfw add 200 deny ip from any to me 25 # telnet localhost 25 Trying 127.0.0.1... And nothing is happening - the connection is neither allowed nor denied, it just hangs. What am I doing wrong? Thanks in advance! From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 14:40:36 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0AB74106566B; Thu, 14 May 2009 14:40:36 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from gizmo.2hip.net (gizmo.2hip.net [64.74.207.195]) by mx1.freebsd.org (Postfix) with ESMTP id A43BD8FC0C; Thu, 14 May 2009 14:40:28 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from [192.168.1.4] (adsl-19-244-249.bna.bellsouth.net [68.19.244.249]) (authenticated bits=0) by gizmo.2hip.net (8.14.3/8.14.3) with ESMTP id n4EEeJrD040260 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Thu, 14 May 2009 10:40:22 -0400 (EDT) (envelope-from rnoland@FreeBSD.org) From: Robert Noland To: "Daniel O'Connor" In-Reply-To: <200905141610.15344.doconnor@gsoft.com.au> References: <20090514030634.GA1252@mooseriver.com> <20090514041834.GB1418@mooseriver.com> <200905141610.15344.doconnor@gsoft.com.au> Content-Type: multipart/signed; micalg="pgp-sha1"; protocol="application/pgp-signature"; boundary="=-8Rd7BVoDQOKluyw8IRZO" Organization: FreeBSD Date: Thu, 14 May 2009 09:39:49 -0500 Message-Id: <1242311989.1755.65.camel@balrog.2hip.net> Mime-Version: 1.0 X-Mailer: Evolution 2.26.1.1 FreeBSD GNOME Team Port X-Spam-Status: No, score=-2.5 required=5.0 tests=AWL,BAYES_00, MIME_QP_LONG_LINE,RDNS_DYNAMIC autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gizmo.2hip.net Cc: freebsd-hackers@freebsd.org, Adrian Chadd , hackers@freebsd.org, Mike Meyer , question@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 14:40:36 -0000 --=-8Rd7BVoDQOKluyw8IRZO Content-Type: text/plain Content-Transfer-Encoding: quoted-printable On Thu, 2009-05-14 at 16:10 +0930, Daniel O'Connor wrote: > On Thu, 14 May 2009, Adrian Chadd wrote: > > 2009/5/14 Josef Grosch : > > > I don't need 2d & 3d acceleration. I just need a card that will > > > handle WindowMaker on a 24 inch Dell monitor at 1920x1200 and as > > > long as the flesh tones on my JPGs don't suck I'm happy. > > > > > > Thanks for the advice. I guess I'm going to make a trip to Fry's > > > Friday. > > > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > > and FreeBSD; let me please point out how sluggish and horribly slow > > it is. >=20 > Depends how unaccelerated it is. >=20 > VESA is pretty damn slow, but even minimal radeon/radeonhd support is=20 > fast enough for desktop use. >=20 > > I gave up trying to get accelerated 3d + dualhead support on the > > card(s) I was using - apparently the hardware just didn't do a single > > viewport span across 2 1280x1024 screens :( > > (The max viewport width was 2048 pixels..) > > > > 2d acceleration may be a must for that kind of resolution.. >=20 > If you have a fast CPU & decent pipe to video memory it isn't necessary,=20 > but very nice. Folks, 2d (EXA) should work on virtually any radeon with 7.2 or 8.0. 3d is currently works on r500 and below. AMD has released preliminary code for 3d on r600+, which I've been working with lately. It isn't ready yet, but it will be soon. If you only need 2d, then Nvidia is also an option. At least if you are ok with running my patch to enable nouveau drm. I've recently managed to get 3d sortof working on NV50 as well, not sure what kind of timeline that will be though, since it is using gallium and isn't as well tested as the old dri code. robert. --=20 Robert Noland FreeBSD --=-8Rd7BVoDQOKluyw8IRZO Content-Type: application/pgp-signature; name="signature.asc" Content-Description: This is a digitally signed message part -----BEGIN PGP SIGNATURE----- Version: GnuPG v2.0.11 (FreeBSD) iEYEABECAAYFAkoMLTUACgkQM4TrQ4qfROPVUACeNZM7QSluX+IA4/KupEHC8A8I 7SMAn3tLncyt6BHxMHkZcljUrxcmUUVu =9XYr -----END PGP SIGNATURE----- --=-8Rd7BVoDQOKluyw8IRZO-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 14:40:36 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0AB74106566B; Thu, 14 May 2009 14:40:36 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from gizmo.2hip.net (gizmo.2hip.net [64.74.207.195]) by mx1.freebsd.org (Postfix) with ESMTP id A43BD8FC0C; Thu, 14 May 2009 14:40:28 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from [192.168.1.4] (adsl-19-244-249.bna.bellsouth.net [68.19.244.249]) (authenticated bits=0) by gizmo.2hip.net (8.14.3/8.14.3) with ESMTP id n4EEeJrD040260 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Thu, 14 May 2009 10:40:22 -0400 (EDT) (envelope-from rnoland@FreeBSD.org) From: Robert Noland To: "Daniel O'Connor" In-Reply-To: <200905141610.15344.doconnor@gsoft.com.au> References: <20090514030634.GA1252@mooseriver.com> <20090514041834.GB1418@mooseriver.com> <200905141610.15344.doconnor@gsoft.com.au> Content-Type: multipart/signed; micalg="pgp-sha1"; protocol="application/pgp-signature"; boundary="=-8Rd7BVoDQOKluyw8IRZO" Organization: FreeBSD Date: Thu, 14 May 2009 09:39:49 -0500 Message-Id: <1242311989.1755.65.camel@balrog.2hip.net> Mime-Version: 1.0 X-Mailer: Evolution 2.26.1.1 FreeBSD GNOME Team Port X-Spam-Status: No, score=-2.5 required=5.0 tests=AWL,BAYES_00, MIME_QP_LONG_LINE,RDNS_DYNAMIC autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gizmo.2hip.net Cc: freebsd-hackers@freebsd.org, Adrian Chadd , hackers@freebsd.org, Mike Meyer , question@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 14:40:36 -0000 --=-8Rd7BVoDQOKluyw8IRZO Content-Type: text/plain Content-Transfer-Encoding: quoted-printable On Thu, 2009-05-14 at 16:10 +0930, Daniel O'Connor wrote: > On Thu, 14 May 2009, Adrian Chadd wrote: > > 2009/5/14 Josef Grosch : > > > I don't need 2d & 3d acceleration. I just need a card that will > > > handle WindowMaker on a 24 inch Dell monitor at 1920x1200 and as > > > long as the flesh tones on my JPGs don't suck I'm happy. > > > > > > Thanks for the advice. I guess I'm going to make a trip to Fry's > > > Friday. > > > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > > and FreeBSD; let me please point out how sluggish and horribly slow > > it is. >=20 > Depends how unaccelerated it is. >=20 > VESA is pretty damn slow, but even minimal radeon/radeonhd support is=20 > fast enough for desktop use. >=20 > > I gave up trying to get accelerated 3d + dualhead support on the > > card(s) I was using - apparently the hardware just didn't do a single > > viewport span across 2 1280x1024 screens :( > > (The max viewport width was 2048 pixels..) > > > > 2d acceleration may be a must for that kind of resolution.. >=20 > If you have a fast CPU & decent pipe to video memory it isn't necessary,=20 > but very nice. Folks, 2d (EXA) should work on virtually any radeon with 7.2 or 8.0. 3d is currently works on r500 and below. AMD has released preliminary code for 3d on r600+, which I've been working with lately. It isn't ready yet, but it will be soon. If you only need 2d, then Nvidia is also an option. At least if you are ok with running my patch to enable nouveau drm. I've recently managed to get 3d sortof working on NV50 as well, not sure what kind of timeline that will be though, since it is using gallium and isn't as well tested as the old dri code. robert. --=20 Robert Noland FreeBSD --=-8Rd7BVoDQOKluyw8IRZO Content-Type: application/pgp-signature; name="signature.asc" Content-Description: This is a digitally signed message part -----BEGIN PGP SIGNATURE----- Version: GnuPG v2.0.11 (FreeBSD) iEYEABECAAYFAkoMLTUACgkQM4TrQ4qfROPVUACeNZM7QSluX+IA4/KupEHC8A8I 7SMAn3tLncyt6BHxMHkZcljUrxcmUUVu =9XYr -----END PGP SIGNATURE----- --=-8Rd7BVoDQOKluyw8IRZO-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 15:05:42 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id D4630106567E for ; Thu, 14 May 2009 15:05:42 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from gizmo.2hip.net (gizmo.2hip.net [64.74.207.195]) by mx1.freebsd.org (Postfix) with ESMTP id 9A91C8FC15; Thu, 14 May 2009 15:05:42 +0000 (UTC) (envelope-from rnoland@FreeBSD.org) Received: from [192.168.1.4] (adsl-19-244-249.bna.bellsouth.net [68.19.244.249]) (authenticated bits=0) by gizmo.2hip.net (8.14.3/8.14.3) with ESMTP id n4EERwYX040196 (version=TLSv1/SSLv3 cipher=DHE-RSA-AES256-SHA bits=256 verify=NO); Thu, 14 May 2009 10:27:58 -0400 (EDT) (envelope-from rnoland@FreeBSD.org) From: Robert Noland To: jgrosch@mooseriver.com In-Reply-To: <20090514030634.GA1252@mooseriver.com> References: <20090514030634.GA1252@mooseriver.com> Content-Type: multipart/signed; micalg="pgp-sha1"; protocol="application/pgp-signature"; boundary="=-DBW8PWtHz1V+SdiKO4EL" Organization: FreeBSD Date: Thu, 14 May 2009 09:27:28 -0500 Message-Id: <1242311248.1755.59.camel@balrog.2hip.net> Mime-Version: 1.0 X-Mailer: Evolution 2.26.1.1 FreeBSD GNOME Team Port X-Spam-Status: No, score=-3.2 required=5.0 tests=AWL,BAYES_00,RDNS_DYNAMIC autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on gizmo.2hip.net Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 15:05:43 -0000 --=-DBW8PWtHz1V+SdiKO4EL Content-Type: text/plain Content-Transfer-Encoding: quoted-printable On Wed, 2009-05-13 at 20:06 -0700, Josef Grosch wrote: > I'm in search for a decent video card. I currently have an Nvidia GeForce > 8400 GS. It worked pretty well i386 FreeBSD 6.2. I have upgraded my home > machine and I am running amd64 FreeBSD 7.2 and it just refuses to go into > X. It just hangs. I've been poking around and, based on what I read, some > FreeBSD developers and Nvidia have gotten into a finger pointing contest = as > to what is the problem. Its all very nice but doesn't help me much. >=20 > So, can any one recommend a good video card? What I'm looking for is >=20 > * Works with amd64 FreeBSD 7.2 > * DVI=20 > * PCI-E x16 > * 512 MB or more > * Not going to cost an arm and a leg >=20 radeon robert. >=20 > Thanks >=20 > Josef --=20 Robert Noland FreeBSD --=-DBW8PWtHz1V+SdiKO4EL Content-Type: application/pgp-signature; name="signature.asc" Content-Description: This is a digitally signed message part -----BEGIN PGP SIGNATURE----- Version: GnuPG v2.0.11 (FreeBSD) iEYEABECAAYFAkoMKlAACgkQM4TrQ4qfROMqewCaA2X64rKm1Q9jraXWPTP5h1R2 tDEAniR+szBhD6LV5+otG9g5XM8K4iHF =N+W+ -----END PGP SIGNATURE----- --=-DBW8PWtHz1V+SdiKO4EL-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 16:06:28 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 9FA7C106566C; Thu, 14 May 2009 16:06:28 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id 71D598FC16; Thu, 14 May 2009 16:06:28 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id 0BC9446B5C; Thu, 14 May 2009 12:06:28 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id D214C8A026; Thu, 14 May 2009 12:06:26 -0400 (EDT) From: John Baldwin To: freebsd-alpha@freebsd.org Date: Thu, 14 May 2009 08:07:35 -0400 User-Agent: KMail/1.9.7 References: <86tz3o4lb9.fsf@ds4.des.no> In-Reply-To: <86tz3o4lb9.fsf@ds4.des.no> MIME-Version: 1.0 Content-Disposition: inline Message-Id: <200905140807.35680.jhb@freebsd.org> Content-Type: text/plain; charset="utf-8" Content-Transfer-Encoding: quoted-printable X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Thu, 14 May 2009 12:06:26 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00, DATE_IN_PAST_03_06,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: Dag-Erling =?utf-8?q?Sm=C3=B8rgrav?= , hackers@freebsd.org Subject: Re: PTE modified bit emulation trap X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 16:06:29 -0000 On Wednesday 13 May 2009 7:47:38 pm Dag-Erling Sm=C3=B8rgrav wrote: > Coverity complains about the lack of error checking in the following > code in sys/kern/kern_sysctl.c, around line 1390: >=20 > /* > * Touch all the wired pages to avoid PTE modified > * bit emulation traps on Alpha while holding locks > * in the sysctl handler. > */ > for (i =3D (wiredlen + PAGE_SIZE - 1) / PAGE_SIZE, > cp =3D req->oldptr; i > 0; i--, cp +=3D PAGE_SIZE) { > copyin(cp, &dummy, 1); > copyout(&dummy, cp, 1); > } >=20 > Since Alpha is dead, can we remove this, or is it still needed for other > platforms? I would check MIPS as it might have similar PTE bits as well (FOR, FOW) (ma= ny=20 Alpha things are similar to MIPS). I don't have my See MIPS Run handy or I= =20 would check it myself. It might be better to replace the loop with a=20 vm_fault(..., VM_FAULT_DIRTY) though if that would have the same effect. =2D-=20 John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 15:16:54 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 1254C106564A for ; Thu, 14 May 2009 15:16:54 +0000 (UTC) (envelope-from mwm@mired.org) Received: from mired.org (two.mired.org [74.143.213.43]) by mx1.freebsd.org (Postfix) with ESMTP id 9D33B8FC1B for ; Thu, 14 May 2009 15:16:52 +0000 (UTC) (envelope-from mwm@mired.org) Received: (qmail 3708 invoked from network); 14 May 2009 10:48:31 -0400 Received: from unknown (HELO ?192.168.195.192?) (192.168.195.192) by 0 with SMTP; 14 May 2009 10:48:31 -0400 From: Mike Meyer To: Adrian Chadd In-Reply-To: X-Mailer: iPhone Mail (5H11) References: <20090514030634.GA1252@mooseriver.com> <20090514000203.3d053800@bhuda.mired.org> <20090514041834.GB1418@mooseriver.com> Message-Id: <6FBF1838-3CB3-41EC-9178-0993EAE3AB84@mired.org> Content-Type: text/plain; charset=us-ascii; format=flowed; delsp=yes Content-Transfer-Encoding: 7bit Mime-Version: 1.0 (iPhone Mail 5H11) Date: Thu, 14 May 2009 10:47:56 -0400 X-Mailman-Approved-At: Thu, 14 May 2009 16:28:29 +0000 Cc: "question@freebsd.org" , "hackers@freebsd.org" Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 15:16:54 -0000 On May 14, 2009, at 1:42, Adrian Chadd wrote: > 2009/5/14 Josef Grosch : > >> I don't need 2d & 3d acceleration. I just need a card that will >> handle >> WindowMaker on a 24 inch Dell monitor at 1920x1200 and as long as >> the flesh >> tones on my JPGs don't suck I'm happy. >> >> Thanks for the advice. I guess I'm going to make a trip to Fry's >> Friday. > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > and FreeBSD; let me please point out how sluggish and horribly slow it > Is. Well, the stock Ubuntu desktop is Gnome, which I find sluggish and horribly slow on amd64 hardware even with Nvidias 2d & 3d acceleration at any size above 1024x768 - at least in it's default config. If all depends on your window manager, config and expectations. Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 82B82106566B for ; Thu, 14 May 2009 16:50:38 +0000 (UTC) (envelope-from des@des.no) Received: from tim.des.no (tim.des.no [194.63.250.121]) by mx1.freebsd.org (Postfix) with ESMTP id 426128FC1E for ; Thu, 14 May 2009 16:50:35 +0000 (UTC) (envelope-from des@des.no) Received: from ds4.des.no (des.no [84.49.246.2]) by smtp.des.no (Postfix) with ESMTP id C62F56D41B; Thu, 14 May 2009 18:50:34 +0200 (CEST) Received: by ds4.des.no (Postfix, from userid 1001) id A6B71844BD; Thu, 14 May 2009 18:50:34 +0200 (CEST) From: =?utf-8?Q?Dag-Erling_Sm=C3=B8rgrav?= To: John Baldwin References: <86tz3o4lb9.fsf@ds4.des.no> <200905140807.35680.jhb@freebsd.org> Date: Thu, 14 May 2009 18:50:34 +0200 In-Reply-To: <200905140807.35680.jhb@freebsd.org> (John Baldwin's message of "Thu, 14 May 2009 08:07:35 -0400") Message-ID: <86preb39yd.fsf@ds4.des.no> User-Agent: Gnus/5.13 (Gnus v5.13) Emacs/23.0.92 (berkeley-unix) MIME-Version: 1.0 Content-Type: text/plain; charset=utf-8 Content-Transfer-Encoding: quoted-printable Cc: hackers@freebsd.org, freebsd-alpha@freebsd.org Subject: Re: PTE modified bit emulation trap X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 16:50:38 -0000 John Baldwin writes: > It might be better to replace the loop with a=20 > vm_fault(..., VM_FAULT_DIRTY) though if that would have the same effect. That was going to be my next question: there must be a more elegant way of doing this :) DES --=20 Dag-Erling Sm=C3=B8rgrav - des@des.no From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 17:32:38 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 0BFDC1065675 for ; Thu, 14 May 2009 17:32:38 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from flat.berklix.org (flat.berklix.org [83.236.223.115]) by mx1.freebsd.org (Postfix) with ESMTP id 87AC88FC1C for ; Thu, 14 May 2009 17:32:33 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from js.berklix.net (p549A4FF8.dip.t-dialin.net [84.154.79.248]) (authenticated bits=0) by flat.berklix.org (8.13.8/8.13.8) with ESMTP id n4EGqYJc009074 for ; Thu, 14 May 2009 18:52:35 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (fire.js.berklix.net [192.168.91.41]) by js.berklix.net (8.13.8/8.13.8) with ESMTP id n4EGqVSd025120 for ; Thu, 14 May 2009 18:52:31 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (localhost [127.0.0.1]) by fire.js.berklix.net (8.14.3/8.14.3) with ESMTP id n4EGr4AW009720 for ; Thu, 14 May 2009 18:53:09 +0200 (CEST) (envelope-from jhs@fire.js.berklix.net) Message-Id: <200905141653.n4EGr4AW009720@fire.js.berklix.net> To: hackers@freebsd.org From: "Julian Stacey" Organization: http://berklix.com BSD Linux Unix Consultancy, Munich Germany. User-agent: EXMH on FreeBSD http://berklix.com/free/ X-URL: http://berklix.com/~jhs/cv/ Date: Thu, 14 May 2009 18:53:04 +0200 Sender: jhs@berklix.org Cc: Subject: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 17:32:38 -0000 Hi hackers@ A commercial firm asked for _Free_ labour today on jobs@freebsd. The censors passed it. Censors of jobs@freebsd.org then blocked the posting below. jobs@ censors again bad, block wrong things, should all be removed & not replaced. Several suckers have already enquired to that firm. Hope we might get some Free labour to donate time to Freebsd, Not Stock holders ! Exact full copy of what Censors blocked: > > ... employer Juniper Networks. ... > > Extra consideration will be given to applicants that can work more > > than 2 hours/day. > > NOTE: This is an unpaid position! > > Juniper Networks is a commercial company, Not a charity. > http://www.juniper.net/us/en/company/investor-relations/#earnings-sec > Unpaid volunteers better working free for FreeBSD > http://freebsdfoundation.org/activities.shtml > A registered charity, > Projects for _Unpaid_ workers > http://wiki.freebsd.org/ > SOC projects > http://www.freebsd.org/news/newsflash.html#event20090510:01 > Some SOC & other projects that didnt get funding would still benefit from > unpaid help. FreeBSD code projects & server admin > would surely love to have an intern donating 2 or more hours a day > free, to benefit FreeBSD globaly, not just Juniper share holders. Cheers, Julian -- Julian Stacey: BSDUnixLinux C Prog Admin SysEng Consult Munich www.berklix.com Mail plain ASCII text. HTML & Base64 text are spam. www.asciiribbon.org From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 18:37:43 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 9EEFF1065692 for ; Thu, 14 May 2009 18:37:43 +0000 (UTC) (envelope-from raysonlogin@gmail.com) Received: from qw-out-2122.google.com (qw-out-2122.google.com [74.125.92.24]) by mx1.freebsd.org (Postfix) with ESMTP id 5AD018FC0A for ; Thu, 14 May 2009 18:37:43 +0000 (UTC) (envelope-from raysonlogin@gmail.com) Received: by qw-out-2122.google.com with SMTP id 3so1033140qwe.7 for ; Thu, 14 May 2009 11:37:42 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:received:in-reply-to:references :date:message-id:subject:from:to:cc:content-type :content-transfer-encoding; bh=ik4LxWvQmtGWtqBK3iAhnQGWXHTmBqhFJxExaQVDs8s=; b=BQjtbKjUht0ma+EWMzu4lCqDe5HRHCQpl9qaIIE3JkoxpGocriI+dFOSInosUwTngV PmUMnIrSjiftt06ZW37+3+gH+yyVJWruXG21AnmikNwVlFwutsymbT5RKLznCnpJ5WJZ JZbBUYlbEW6UDDe9unpNEOQ+cLumaO8+jH5k8= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:in-reply-to:references:date:message-id:subject:from:to :cc:content-type:content-transfer-encoding; b=tw/NksTbCNxQxpWLUADI1nDwLovP2E6CZ17aDWEz8RCaJf6pi3UKxCj9z3Za/v24/j JajO6X5VLWdtJszw9HH7tLx/5q46DmDqrfqRuP1XYGiStX2noIvQLu9pXtH+DF4PTp/7 Zt4nPt5LYKWiPEZtineckpZ+jd7J1FAroEhO0= MIME-Version: 1.0 Received: by 10.229.96.10 with SMTP id f10mr1747017qcn.72.1242324918615; Thu, 14 May 2009 11:15:18 -0700 (PDT) In-Reply-To: <200905141653.n4EGr4AW009720@fire.js.berklix.net> References: <200905141653.n4EGr4AW009720@fire.js.berklix.net> Date: Thu, 14 May 2009 13:15:18 -0500 Message-ID: <73a01bf20905141115s8fffdc3t12060c82982e5812@mail.gmail.com> From: Rayson Ho To: Julian Stacey Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: 7bit Cc: hackers@freebsd.org, alfred@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 18:37:43 -0000 Thanks for letting us know! I am sure at least a few of us here will buy less products from Juniper Networks. Rayson On Thu, May 14, 2009 at 11:53 AM, Julian Stacey wrote: > Hi hackers@ > A commercial firm asked for _Free_ labour today on jobs@freebsd. > The censors passed it. Censors of jobs@freebsd.org then blocked > the posting below. jobs@ censors again bad, block wrong things, > should all be removed & not replaced. > > Several suckers have already enquired to that firm. Hope we might get > some Free labour to donate time to Freebsd, Not Stock holders ! > > Exact full copy of what Censors blocked: >> > ... employer Juniper Networks. ... >> > Extra consideration will be given to applicants that can work more >> > than 2 hours/day. >> > NOTE: This is an unpaid position! >> >> Juniper Networks is a commercial company, Not a charity. >> http://www.juniper.net/us/en/company/investor-relations/#earnings-sec >> Unpaid volunteers better working free for FreeBSD >> http://freebsdfoundation.org/activities.shtml >> A registered charity, >> Projects for _Unpaid_ workers >> http://wiki.freebsd.org/ >> SOC projects >> http://www.freebsd.org/news/newsflash.html#event20090510:01 >> Some SOC & other projects that didnt get funding would still benefit from >> unpaid help. FreeBSD code projects & server admin >> would surely love to have an intern donating 2 or more hours a day >> free, to benefit FreeBSD globaly, not just Juniper share holders. > > Cheers, > Julian > -- > Julian Stacey: BSDUnixLinux C Prog Admin SysEng Consult Munich www.berklix.com > Mail plain ASCII text. HTML & Base64 text are spam. www.asciiribbon.org > _______________________________________________ > freebsd-hackers@freebsd.org mailing list > http://lists.freebsd.org/mailman/listinfo/freebsd-hackers > To unsubscribe, send any mail to "freebsd-hackers-unsubscribe@freebsd.org" > From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 18:46:06 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id B60ED1065672 for ; Thu, 14 May 2009 18:46:06 +0000 (UTC) (envelope-from mattjeet@gmail.com) Received: from mail-px0-f106.google.com (mail-px0-f106.google.com [209.85.216.106]) by mx1.freebsd.org (Postfix) with ESMTP id 892028FC16 for ; Thu, 14 May 2009 18:46:06 +0000 (UTC) (envelope-from mattjeet@gmail.com) Received: by pxi4 with SMTP id 4so800387pxi.3 for ; Thu, 14 May 2009 11:46:06 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:mime-version:sender:reply-to:received :in-reply-to:references:date:x-google-sender-auth:message-id:subject :from:to:cc:content-type:content-transfer-encoding; bh=vkZqi86NFJavox6oYN9sPhGiYZKaurudowrCoo4eKlo=; b=EUkGTeJSLBffcoBVlwPYbqzCKJAdu/SReajPnG+fUOW82P1/XrWIfmebCvqbOUOLjM Br0A1bIWmIIc/S2mW1HEgPvahJbt/hU0I+hZwepq4eUDVK3fkRDzg7zIi6AvRivoX7Dq pXaLsq2vs44BYl1O0W6Ed9MqBfDOo+Efc5Mhc= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=mime-version:sender:reply-to:in-reply-to:references:date :x-google-sender-auth:message-id:subject:from:to:cc:content-type :content-transfer-encoding; b=h4v9u/Mt/Nwn7UEd0mUx8vYlaI2Mb2W5weiIN8g+LoKIFTRg0y1IGIfD+ojwTK0st5 wHz1l87ZaOroEa4Q5YSxnzau2uZq3pfCsDk9Btawjdy7U6kXYVDEBgIzibHxTeZdtLck /gPI5Y/HLHPlXC6O3F35hudIZehzD3I+zvCnc= MIME-Version: 1.0 Sender: mattjeet@gmail.com Received: by 10.142.49.20 with SMTP id w20mr794323wfw.278.1242325178933; Thu, 14 May 2009 11:19:38 -0700 (PDT) In-Reply-To: <200905141653.n4EGr4AW009720@fire.js.berklix.net> References: <200905141653.n4EGr4AW009720@fire.js.berklix.net> Date: Thu, 14 May 2009 11:19:38 -0700 X-Google-Sender-Auth: 18ca4b23306f1d39 Message-ID: <9740caf0905141119o193eda9h1bde4dbbb8f8645e@mail.gmail.com> From: Matt Olander To: Julian Stacey Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: matt@ixsystems.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 18:46:07 -0000 On Thu, May 14, 2009 at 9:53 AM, Julian Stacey wrote: > Hi hackers@ > A commercial firm asked for _Free_ labour today on jobs@freebsd. > The censors passed it. =A0Censors of jobs@freebsd.org then blocked > the posting below. =A0jobs@ censors again bad, block wrong things, > should all be removed & not replaced. > > Several suckers have already enquired to that firm. =A0Hope we might get > some Free labour to donate time to Freebsd, Not Stock holders ! Hi Julian, Internships are an accepted way for a high school or university student (and nowadays some post grad students and others) to gain a bit of experience in their field before joining the work force or perhaps while switching careers. At my company, we've filled several full-time positions with people that were interns first. It's just a way to fill a part-time, sometimes non-paid job, at a company where there isn't an official requisition for that particular position. Nobody is forcing anybody to take the internship and it is clearly stated that it is a non-paid internship in the post. I imagine that there would be some interested students or unemployed people that would love to work with Alfred on a project at Juniper a few hours a week in their spare time, for free. It will look great on a resume, they will probably learn some valuable skills, and perhaps parlay it into a full-time, paid position. best, -matt > > Exact full copy of what Censors blocked: >> > ... employer Juniper Networks. ... >> > Extra consideration will be given to applicants that can work more >> > than 2 hours/day. >> > NOTE: This is an unpaid position! >> >> Juniper Networks is a commercial company, Not a charity. >> =A0 =A0 =A0 http://www.juniper.net/us/en/company/investor-relations/#ear= nings-sec >> Unpaid volunteers better working free for FreeBSD >> =A0 =A0 =A0 http://freebsdfoundation.org/activities.shtml >> =A0 =A0 =A0 A registered charity, >> Projects for _Unpaid_ workers >> =A0 =A0 =A0 http://wiki.freebsd.org/ >> SOC projects >> =A0 =A0 =A0 http://www.freebsd.org/news/newsflash.html#event20090510:01 >> Some SOC & other projects that didnt get funding would still benefit fro= m >> unpaid help. =A0FreeBSD code projects & server admin >> would surely love to have an intern donating 2 or more hours a day >> free, to benefit FreeBSD globaly, not just Juniper share holders. > > Cheers, > Julian > -- > Julian Stacey: BSDUnixLinux C Prog Admin SysEng Consult Munich www.berkli= x.com > =A0Mail plain ASCII text. =A0HTML & Base64 text are spam. www.asciiribbon= .org > _______________________________________________ > freebsd-hackers@freebsd.org mailing list > http://lists.freebsd.org/mailman/listinfo/freebsd-hackers > To unsubscribe, send any mail to "freebsd-hackers-unsubscribe@freebsd.org= " > From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 19:25:08 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 4747C1065670 for ; Thu, 14 May 2009 19:25:08 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: from kiwi-computer.com (keira.kiwi-computer.com [63.224.10.3]) by mx1.freebsd.org (Postfix) with SMTP id CE6C98FC1A for ; Thu, 14 May 2009 19:25:07 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: (qmail 45251 invoked by uid 2001); 14 May 2009 18:58:26 -0000 Date: Thu, 14 May 2009 13:58:26 -0500 From: "Rick C. Petty" To: Josef Grosch Message-ID: <20090514185826.GA45111@keira.kiwi-computer.com> References: <20090514030634.GA1252@mooseriver.com> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <20090514030634.GA1252@mooseriver.com> User-Agent: Mutt/1.4.2.3i Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: rick-freebsd2008@kiwi-computer.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 19:25:14 -0000 On Wed, May 13, 2009 at 08:06:34PM -0700, Josef Grosch wrote: > > So, can any one recommend a good video card? What I'm looking for is > > * Works with amd64 FreeBSD 7.2 > * DVI > * PCI-E x16 > * 512 MB or more > * Not going to cost an arm and a leg I just bought an nVidia and an ATI on newegg for under $30 each (plus mail-in rebates), buth PCI x16, DVI+VGA, 512MB. I have tried them both on amd64 and this is what I've discovered: - The ATI is quite fast for xvideo (via mplayer) and somewhat fast on 3D, there seems to be some cursor-related artifacts (I've tried a number of cards with the same results). - The nVidia card required Robert Noland's patches applied against RELENG_7, and the latest git checkouts of the nouveau driver and the libdrm code. I forcibly installed xf86-video-nouveau and then "gmake install"'d the nouveau build on top of it. I did the same for libdrm. It was very slow for xvideo (mplayer) and 3D acceleration was nonexistent. I could not get the "nv" driver to work in dual-head mode nor in single-head mode. Nouveau didn't support my onboard card either. Neither of these drivers comes remotely close to the performance of the same cards using the nvidia driver (on i386). I tried ati and nouveau on i386 for comparisons. The nvidia driver did support my onboard video. I ran these tests on a couple of ATI cards and various nvidia cards. It was very frustrating. I'm using the ati/radeon driver currently on amd64 until nvidia finishes their 64-bit driver. YMMV, -- Rick C. Petty From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 19:27:07 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 2B8E11065674 for ; Thu, 14 May 2009 19:27:07 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: from kiwi-computer.com (keira.kiwi-computer.com [63.224.10.3]) by mx1.freebsd.org (Postfix) with SMTP id B3AEE8FC25 for ; Thu, 14 May 2009 19:27:06 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: (qmail 45317 invoked by uid 2001); 14 May 2009 19:00:25 -0000 Date: Thu, 14 May 2009 14:00:25 -0500 From: "Rick C. Petty" To: Adrian Chadd Message-ID: <20090514190025.GB45111@keira.kiwi-computer.com> References: <20090514030634.GA1252@mooseriver.com> <20090514000203.3d053800@bhuda.mired.org> <20090514041834.GB1418@mooseriver.com> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: User-Agent: Mutt/1.4.2.3i Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: rick-freebsd2008@kiwi-computer.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 19:27:07 -0000 On Thu, May 14, 2009 at 01:42:20PM +0800, Adrian Chadd wrote: > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > and FreeBSD; let me please point out how sluggish and horribly slow it > is. > > I gave up trying to get accelerated 3d + dualhead support on the > card(s) I was using - apparently the hardware just didn't do a single > viewport span across 2 1280x1024 screens :( > (The max viewport width was 2048 pixels..) With the nvidia driver I've seen great 3d acceleration work on both heads without using twinview (because I want different resolutions on each head). Perhaps the ATI hardware isn't capable of this, but nvidia's cards seem to be. It's too bad the open source drivers haven't made enough progress in this area yet. -- Rick C. Petty From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 19:28:55 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 2797710656A6 for ; Thu, 14 May 2009 19:28:55 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: from kiwi-computer.com (keira.kiwi-computer.com [63.224.10.3]) by mx1.freebsd.org (Postfix) with SMTP id B28828FC1D for ; Thu, 14 May 2009 19:28:54 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: (qmail 45341 invoked by uid 2001); 14 May 2009 19:02:13 -0000 Date: Thu, 14 May 2009 14:02:13 -0500 From: "Rick C. Petty" To: Daniel O'Connor Message-ID: <20090514190213.GC45111@keira.kiwi-computer.com> References: <20090514030634.GA1252@mooseriver.com> <20090514041834.GB1418@mooseriver.com> <200905141610.15344.doconnor@gsoft.com.au> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <200905141610.15344.doconnor@gsoft.com.au> User-Agent: Mutt/1.4.2.3i Cc: freebsd-hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: rick-freebsd2008@kiwi-computer.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 19:28:55 -0000 On Thu, May 14, 2009 at 04:10:07PM +0930, Daniel O'Connor wrote: > > Depends how unaccelerated it is. > > VESA is pretty damn slow, but even minimal radeon/radeonhd support is > fast enough for desktop use. VESA doesn't support dual-head, if that's something you're looking for. And I agree that it's particularly slow even in 2d. -- Rick C. Petty From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 20:00:27 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id E98E11065670 for ; Thu, 14 May 2009 20:00:27 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: from kiwi-computer.com (keira.kiwi-computer.com [63.224.10.3]) by mx1.freebsd.org (Postfix) with SMTP id 7FC0E8FC12 for ; Thu, 14 May 2009 20:00:27 +0000 (UTC) (envelope-from rick@kiwi-computer.com) Received: (qmail 45317 invoked by uid 2001); 14 May 2009 19:00:25 -0000 Date: Thu, 14 May 2009 14:00:25 -0500 From: "Rick C. Petty" To: Adrian Chadd Message-ID: <20090514190025.GB45111@keira.kiwi-computer.com> References: <20090514030634.GA1252@mooseriver.com> <20090514000203.3d053800@bhuda.mired.org> <20090514041834.GB1418@mooseriver.com> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: User-Agent: Mutt/1.4.2.3i Cc: question@freebsd.org, hackers@freebsd.org Subject: Re: In search of a video card X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list Reply-To: rick-freebsd2008@kiwi-computer.com List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 20:00:28 -0000 On Thu, May 14, 2009 at 01:42:20PM +0800, Adrian Chadd wrote: > > I've experienced no-acceleration radeon driver "desktop" under Ubuntu > and FreeBSD; let me please point out how sluggish and horribly slow it > is. > > I gave up trying to get accelerated 3d + dualhead support on the > card(s) I was using - apparently the hardware just didn't do a single > viewport span across 2 1280x1024 screens :( > (The max viewport width was 2048 pixels..) With the nvidia driver I've seen great 3d acceleration work on both heads without using twinview (because I want different resolutions on each head). Perhaps the ATI hardware isn't capable of this, but nvidia's cards seem to be. It's too bad the open source drivers haven't made enough progress in this area yet. -- Rick C. Petty From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 21:34:27 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 79643106564A; Thu, 14 May 2009 21:34:27 +0000 (UTC) (envelope-from ed@hoeg.nl) Received: from palm.hoeg.nl (mx0.hoeg.nl [IPv6:2001:7b8:613:100::211]) by mx1.freebsd.org (Postfix) with ESMTP id 3DAEF8FC13; Thu, 14 May 2009 21:34:27 +0000 (UTC) (envelope-from ed@hoeg.nl) Received: by palm.hoeg.nl (Postfix, from userid 1000) id 9E5381D17D; Thu, 14 May 2009 23:34:26 +0200 (CEST) Date: Thu, 14 May 2009 23:34:26 +0200 From: Ed Schouten To: John Baldwin Message-ID: <20090514213426.GP58540@hoeg.nl> References: <200905111224.26856.jhb@freebsd.org> <200905111801.18767.jhb@freebsd.org> MIME-Version: 1.0 Content-Type: multipart/signed; micalg=pgp-sha1; protocol="application/pgp-signature"; boundary="FbCNvfVkhudvi8fu" Content-Disposition: inline In-Reply-To: <200905111801.18767.jhb@freebsd.org> User-Agent: Mutt/1.5.19 (2009-01-05) Cc: FreeBSD Hackers , jt@0xabadba.be Subject: Re: concurrent sysctl implementation X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 21:34:27 -0000 --FbCNvfVkhudvi8fu Content-Type: text/plain; charset=us-ascii Content-Disposition: inline Content-Transfer-Encoding: quoted-printable * John Baldwin wrote: > Well, in theory a bunch of "small" requests to SYSCTL_PROC() nodes that u= sed=20 > sysctl_wire_old() (or whatever it is called) could cause the amount of us= er=20 > memory wired for sysctls to grow unbounded. Thus, allowing this limited= =20 > concurrency is a tradeoff as there is a minimal (perhaps only theoretical= at=20 > the moment) risk of removing the safety net. >=20 > The patch is quite small, btw, because the locking for the sysctl tree al= ready=20 > exists, and by using read locks, one can already allow concurrent sysctl= =20 > requests. There is no need to add any new locks or restructure the sysct= l=20 > tree, just to adjust the locking that is already present. It might be=20 > clearer, in fact, to split the sysctl memory lock back out into a separat= e=20 > lock. This would allow "small" sysctl requests to run concurrently with = a=20 > single "large" request whereas in my suggestion in the earlier e-mail,=20 > the "large" request will block all other user requests until it finishes. >=20 > I've actually gone ahead and done this below. Boohoo. I actually wanted jt to work on this, as a small exercise to figure out the way locking primitives work in the kernel. No problem, because I can think of dozens of other things. Is there a chance we can see this patch in 8.0? I like it that the memlock is being picked up before we pick up the sysctl lock itself, which makes a lot of sense. --=20 Ed Schouten WWW: http://80386.nl/ --FbCNvfVkhudvi8fu Content-Type: application/pgp-signature Content-Disposition: inline -----BEGIN PGP SIGNATURE----- Version: GnuPG v1.4.9 (FreeBSD) iEYEARECAAYFAkoMjmIACgkQ52SDGA2eCwW0hACbB/4W3DshwsRPIuaXta+Wl8IX Y34An1UveDTp8oQMQb8jOCiMAgaTk2ve =vX/X -----END PGP SIGNATURE----- --FbCNvfVkhudvi8fu-- From owner-freebsd-hackers@FreeBSD.ORG Thu May 14 21:58:21 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 14D001065679 for ; Thu, 14 May 2009 21:58:21 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from cyrus.watson.org (cyrus.watson.org [65.122.17.42]) by mx1.freebsd.org (Postfix) with ESMTP id DAA6E8FC1A for ; Thu, 14 May 2009 21:58:20 +0000 (UTC) (envelope-from jhb@freebsd.org) Received: from bigwig.baldwin.cx (66.111.2.69.static.nyinternet.net [66.111.2.69]) by cyrus.watson.org (Postfix) with ESMTPSA id 8F9D846B0C; Thu, 14 May 2009 17:58:20 -0400 (EDT) Received: from jhbbsd.hudson-trading.com (unknown [209.249.190.8]) by bigwig.baldwin.cx (Postfix) with ESMTPA id 76FED8A025; Thu, 14 May 2009 17:58:14 -0400 (EDT) From: John Baldwin To: Ed Schouten Date: Thu, 14 May 2009 17:57:51 -0400 User-Agent: KMail/1.9.7 References: <200905111801.18767.jhb@freebsd.org> <20090514213426.GP58540@hoeg.nl> In-Reply-To: <20090514213426.GP58540@hoeg.nl> MIME-Version: 1.0 Content-Type: text/plain; charset="iso-8859-1" Content-Transfer-Encoding: 7bit Content-Disposition: inline Message-Id: <200905141757.52144.jhb@freebsd.org> X-Greylist: Sender succeeded SMTP AUTH, not delayed by milter-greylist-4.0.1 (bigwig.baldwin.cx); Thu, 14 May 2009 17:58:14 -0400 (EDT) X-Virus-Scanned: clamav-milter 0.95 at bigwig.baldwin.cx X-Virus-Status: Clean X-Spam-Status: No, score=-2.5 required=4.2 tests=AWL,BAYES_00,RDNS_NONE autolearn=no version=3.2.5 X-Spam-Checker-Version: SpamAssassin 3.2.5 (2008-06-10) on bigwig.baldwin.cx Cc: FreeBSD Hackers , jt@0xabadba.be Subject: Re: concurrent sysctl implementation X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Thu, 14 May 2009 21:58:21 -0000 On Thursday 14 May 2009 5:34:26 pm Ed Schouten wrote: > * John Baldwin wrote: > > Well, in theory a bunch of "small" requests to SYSCTL_PROC() nodes that used > > sysctl_wire_old() (or whatever it is called) could cause the amount of user > > memory wired for sysctls to grow unbounded. Thus, allowing this limited > > concurrency is a tradeoff as there is a minimal (perhaps only theoretical at > > the moment) risk of removing the safety net. > > > > The patch is quite small, btw, because the locking for the sysctl tree already > > exists, and by using read locks, one can already allow concurrent sysctl > > requests. There is no need to add any new locks or restructure the sysctl > > tree, just to adjust the locking that is already present. It might be > > clearer, in fact, to split the sysctl memory lock back out into a separate > > lock. This would allow "small" sysctl requests to run concurrently with a > > single "large" request whereas in my suggestion in the earlier e-mail, > > the "large" request will block all other user requests until it finishes. > > > > I've actually gone ahead and done this below. > > Boohoo. I actually wanted jt to work on this, as a small exercise to > figure out the way locking primitives work in the kernel. No problem, > because I can think of dozens of other things. > > Is there a chance we can see this patch in 8.0? I like it that the > memlock is being picked up before we pick up the sysctl lock itself, > which makes a lot of sense. Yes, I can commit it. -- John Baldwin From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 05:51:35 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 37C9D1065694 for ; Fri, 15 May 2009 05:51:35 +0000 (UTC) (envelope-from kheuer2@gwdg.de) Received: from tmailer.gwdg.de (tmailer.gwdg.de [134.76.10.23]) by mx1.freebsd.org (Postfix) with ESMTP id C17A78FC0C for ; Fri, 15 May 2009 05:51:34 +0000 (UTC) (envelope-from kheuer2@gwdg.de) Received: from gwdu60.gwdg.de ([134.76.8.60]) by mailer.gwdg.de with esmtps (TLSv1:AES256-SHA:256) (Exim 4.69) (envelope-from ) id 1M4qKT-0001vT-Bw; Fri, 15 May 2009 07:51:33 +0200 Date: Fri, 15 May 2009 07:51:33 +0200 (CEST) From: Konrad Heuer To: Robert Watson In-Reply-To: Message-ID: <20090515073949.M70549@gwdu60.gwdg.de> References: <20090508101555.J47014@gwdu60.gwdg.de> MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed X-Spam-Level: - X-Virus-Scanned: (clean) by exiscan+sophie Cc: freebsd-hackers@freebsd.org Subject: Re: How to invalidate NFS read cache? X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 05:51:35 -0000 On Tue, 12 May 2009, Robert Watson wrote: > On Fri, 8 May 2009, Konrad Heuer wrote: > >> sporadically, I observe a strange but serious problem in our large NFS >> environment. NFS servers are Linux and OS X with StorNext/Xsan cluster >> filesystems, NFS clients Linux and FreeBSD. >> >> NFS client A changes a file, but nfs client B (running on FreeBSD) does >> still see the old version. On the NFS server itself, everything looks fine. >> >> Afaik the FreeBSD kernel invalidates the NFS read cache if file >> modification time on the server changed which should happen here but >> doesn't. Can I force FreeBSD (e.g. by sysctl setting) to read file buffers >> again unconditionally after vfs.nfs.access_cache_timeout seconds have >> passed? > > Hi Konrad: > > Normally, NFS clients implement open-to-close consistency, which dictates > that when a close() occurs on client A, all pending writes on the file should > be issued to the server before close() returns, so that a signal to client B > to open() the file can validate its cache before open() returns. > > This raises the following question: is client A closing the file, and is > client B then opening it? > > If not: relying on writes being visible on the client B before the close() on > A and a fresh open() on B is not guaranteed to work, although we can discuss > ways to improve behavior with respect to expectation. Try modifying your > application and see if it gets the desired behavior, and then we can discuss > ways to improve what you're seeing. > > If you are: this is probably a bug in our caching and or issuing of NFS RPCs. > We cache both attribute and access data -- perhaps there is an open() path > where we issue neither RPC? In the case of open, we likely should test for a > valid access cache entry, and if there is one, issue an attribute read, and > otherwise just issue an access check which will piggyback fresh attribute > data on the reply. Perhaps there is a bug here somewhere. > > A few other misc questions: > > - Could you confirm you're using NFSv3 on all clients. Are there any special > mount options in use? > - What version of FreeBSD are you running with? > > In FreeBSD 8.x, we now have DTrace probes for all of the above events -- > VOPs, attribute cache hit/miss/load/flush, access cache hit/miss/load/flush, > RPCs, etc, which we can use to debug the problem. I haven't yet MFC'd these > to 7.x, but if you're able to run a very fresh 7-STABLE, I can probably > produce a patch to add it for you in a few days. Hello, Robert, thank you very much for your reply! The problem I observe happens with FreeBSD 6.4-R and 7.0-R with nfsv3. The fstab entry I use is: server:/Volume /local/dir nfs bg,rw,intr,-T,-r32768,-w16384 0 0 The server runs on Mac OSX 10.5. In the meantime, I had the chance to examine a failure a little bit closer. As far as I can see in the moment a file modified on a Linux NFS client gets a new modification time on the NFS server but the FreeBSD client still sees the old timestamp. This obviously happens sporadically only under some circumstances I do not know further. I'll do some further testing the next days. Could you imagine a kind of directory or metadata caching on FreeBSD NFS clients that may cause this behaviour? Best regards Konrad Konrad Heuer GWDG, Am Fassberg, 37077 Goettingen, Germany, kheuer2@gwdg.de From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 07:34:47 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id F19831065670; Fri, 15 May 2009 07:34:47 +0000 (UTC) (envelope-from kheuer2@gwdg.de) Received: from tmailer.gwdg.de (tmailer.gwdg.de [134.76.10.23]) by mx1.freebsd.org (Postfix) with ESMTP id B32E58FC1B; Fri, 15 May 2009 07:34:47 +0000 (UTC) (envelope-from kheuer2@gwdg.de) Received: from gwdu60.gwdg.de ([134.76.8.60]) by mailer.gwdg.de with esmtps (TLSv1:AES256-SHA:256) (Exim 4.69) (envelope-from ) id 1M4rwM-00044K-7b; Fri, 15 May 2009 09:34:46 +0200 Date: Fri, 15 May 2009 09:34:46 +0200 (CEST) From: Konrad Heuer To: Robert Watson In-Reply-To: <20090515073949.M70549@gwdu60.gwdg.de> Message-ID: <20090515093121.W70549@gwdu60.gwdg.de> References: <20090508101555.J47014@gwdu60.gwdg.de> <20090515073949.M70549@gwdu60.gwdg.de> MIME-Version: 1.0 Content-Type: TEXT/PLAIN; charset=US-ASCII; format=flowed X-Spam-Level: - X-Virus-Scanned: (clean) by exiscan+sophie Cc: freebsd-hackers@freebsd.org Subject: Re: How to invalidate NFS read cache? X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 07:34:48 -0000 On Fri, 15 May 2009, Konrad Heuer wrote: > (...) > The problem I observe happens with FreeBSD 6.4-R and 7.0-R with nfsv3. The > fstab entry I use is: > > server:/Volume /local/dir nfs bg,rw,intr,-T,-r32768,-w16384 0 0 > > The server runs on Mac OSX 10.5. > > In the meantime, I had the chance to examine a failure a little bit closer. > As far as I can see in the moment a file modified on a Linux NFS client gets > a new modification time on the NFS server but the FreeBSD client still sees > the old timestamp. This obviously happens sporadically only under some > circumstances I do not know further. I'll do some further testing the next > days. > > Could you imagine a kind of directory or metadata caching on FreeBSD NFS > clients that may cause this behaviour? I forgot to mention one detail: File modification happens with emacs; thus the modified file is indeed a new one with a new inode number whereas the old version keeps its inode and gets renamed. Best regards Konrad Konrad Heuer GWDG, Am Fassberg, 37077 Goettingen, Germany, kheuer2@gwdg.de From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 11:48:52 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id ACC34106566C for ; Fri, 15 May 2009 11:48:52 +0000 (UTC) (envelope-from marius@nuenneri.ch) Received: from mail-gx0-f172.google.com (mail-gx0-f172.google.com [209.85.217.172]) by mx1.freebsd.org (Postfix) with ESMTP id 73CA88FC08 for ; Fri, 15 May 2009 11:48:52 +0000 (UTC) (envelope-from marius@nuenneri.ch) Received: by gxk20 with SMTP id 20so1465019gxk.19 for ; Fri, 15 May 2009 04:48:51 -0700 (PDT) MIME-Version: 1.0 Received: by 10.151.135.12 with SMTP id m12mr5848630ybn.70.1242388131831; Fri, 15 May 2009 04:48:51 -0700 (PDT) In-Reply-To: <814ovqn8dp.fsf@zhuzha.ua1> References: <814ovqn8dp.fsf@zhuzha.ua1> Date: Fri, 15 May 2009 13:48:51 +0200 Message-ID: From: =?ISO-8859-1?Q?Marius_N=FCnnerich?= To: Mikolaj Golub Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org Subject: Re: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 11:48:52 -0000 On Tue, May 12, 2009 at 08:27, Mikolaj Golub wrot= e: > Hi, > > The code below is compiled with -fopenmp and run on FreeBSD6/7 (i386, amd= 64): > > #include > #include > > int n =3D 4, m =3D 2; > > int main () { > =A0 =A0 =A0 =A0for (;;) { > =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0int i; > > =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); > #pragma omp parallel for num_threads(m) > =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} > > =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); > #pragma omp parallel for num_threads(n) > =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} > > =A0 =A0 =A0 =A0} > > =A0 =A0 =A0 =A0return 0; > } > > During the run the program's virtual memory usage constantly grows. The g= rowth > is observed only when n !=3D m. When running the program with uncommented > sleep() and observing the number of threads with 'top -H' I see in turn 2= or 4 > threads. So it looks like memory leak when thread is removed. Should I fi= ll > PR? I can confirm this. I briefly looked through the libgomp code but didn't see the leak. Anybody knows good tools how to investigate this? From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 13:18:25 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 526741065670 for ; Fri, 15 May 2009 13:18:25 +0000 (UTC) (envelope-from andrit@ukr.net) Received: from emailsecurity-del1-1.globallogic.com (mx-del1-1.globallogic.com [202.174.92.25]) by mx1.freebsd.org (Postfix) with ESMTP id DD4918FC17 for ; Fri, 15 May 2009 13:18:19 +0000 (UTC) (envelope-from andrit@ukr.net) Received: from emailsecurity-del1-1.globallogic.com (127.0.0.1) by emailsecurity-del1-1.globallogic.com (MlfMTA v3.2r9) id h1lln40171so for ; Fri, 15 May 2009 18:32:27 +0530 (envelope-from ) Received: from EX2-KBP1.synapse.com ([172.17.48.26]) by emailsecurity-del1-1.globallogic.com (SonicWALL 7.1.0.1801) with ESMTP; Fri, 15 May 2009 18:32:18 +0530 Received: from [172.17.58.168] ([172.17.58.168]) by EX2-KBP1.synapse.com with Microsoft SMTPSVC(6.0.3790.3959); Fri, 15 May 2009 16:02:49 +0300 Message-ID: <4A0D67D8.8070401@ukr.net> Date: Fri, 15 May 2009 16:02:16 +0300 From: Andriy Tkachuk User-Agent: Thunderbird 2.0.0.21 (Windows/20090302) MIME-Version: 1.0 To: =?ISO-8859-1?Q?Marius_N=FCnnerich?= References: <814ovqn8dp.fsf@zhuzha.ua1> In-Reply-To: Content-Type: text/plain; charset=ISO-8859-1; format=flowed Content-Transfer-Encoding: 8bit X-OriginalArrivalTime: 15 May 2009 13:02:49.0425 (UTC) FILETIME=[72F73C10:01C9D55D] X-Mlf-Version: 7.1.0.1801 X-Mlf-UniqueId: o200905151302170038848 Cc: freebsd-hackers@freebsd.org, Mikolaj Golub Subject: Re: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 13:18:25 -0000 On 2009-05-15 14:48, Marius Nünnerich wrote: > Anybody knows good tools how to investigate this? Valgrind? From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 14:42:57 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id DE49E106564A for ; Fri, 15 May 2009 14:42:57 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from flat.berklix.org (flat.berklix.org [83.236.223.115]) by mx1.freebsd.org (Postfix) with ESMTP id 48B6D8FC0C for ; Fri, 15 May 2009 14:42:56 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from js.berklix.net (p549A4424.dip.t-dialin.net [84.154.68.36]) (authenticated bits=0) by flat.berklix.org (8.13.8/8.13.8) with ESMTP id n4FEgpft025740; Fri, 15 May 2009 16:42:53 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (fire.js.berklix.net [192.168.91.41]) by js.berklix.net (8.13.8/8.13.8) with ESMTP id n4FEgR9t011506; Fri, 15 May 2009 16:42:27 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (localhost [127.0.0.1]) by fire.js.berklix.net (8.14.3/8.14.3) with ESMTP id n4FEh9Tf027120; Fri, 15 May 2009 16:43:14 +0200 (CEST) (envelope-from jhs@fire.js.berklix.net) Message-Id: <200905151443.n4FEh9Tf027120@fire.js.berklix.net> To: matt@ixsystems.com From: "Julian Stacey" Organization: http://berklix.com BSD Unix Linux Consultancy, Munich Germany User-agent: EXMH on FreeBSD http://berklix.com/free/ X-URL: http://berklix.com In-reply-to: Your message "Thu, 14 May 2009 11:19:38 PDT." <9740caf0905141119o193eda9h1bde4dbbb8f8645e@mail.gmail.com> Date: Fri, 15 May 2009 16:43:09 +0200 Sender: jhs@berklix.org Cc: hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 14:42:58 -0000 Hi Matt, > > Several suckers have already enquired to that firm. =A0Hope we might get > > some Free labour to donate time to Freebsd, Not Stock holders ! > > Hi Julian, > Internships are an accepted way for a high school or university In America. America imported unpaid apprenticeships & indentured servitude (time limited slavery) from Europe/Britain centuries ago. Britain dumped both Long since. (Germany still has some interns eg in theatre, last described as a rip off). Condolences that the "Land of the free" retains medieval European intern practice. > it is clearly stated that it is a non-paid internship in the post. Not clear at start. The word "intern" may be clear warning of No Money in American dialect, but to British eyes, it was a strange word out of context & ignored. ( Monika Lewinsky news first brought the quaint old fashioned American word & concept of Intern back across the Atlantic, but in English, Intern just means certain some workers ). Posting near end had: "San Francisco" Posting in final line had: "This is an unpaid position!" Posting should have started "USA/ San Francisco - Unpaid job" to efficiently enable global readership of jobs@ to delete unread, but American-centric censors of global jobs@ messed up as often, > I imagine that there would be some interested students or unemployed > people that would love to work with Alfred on a project at Juniper a > few hours a week in their spare time, for free. http://lists.freebsd.org/pipermail/freebsd-jobs/2009-May/000652.html "more than 2 hours/day" That's 1/4 or more of a full time job - _Unpaid_ ! No offer of money, food, transport, training courses, books, hardware to keep. It undermines labour rates for all BSD workers. The jobs@freebsd.org censors blocked my polite post people instead work free for freebsd.org > It will look great on > a resume, they will probably learn some valuable skills, and perhaps > parlay it into a full-time, paid position. Managers will read: "This keen sucker can be kept at Low rates for a Long time". Better that FreeBSD people work free Not for scrounging commercial firms & share holder profit, but for charity eg: FreeBSD development projects & systems admin (eg send-pr base, (parlay into a job requiring corporate support/ trouble ticket experience ), FSF, Xorg, Greenpeace, computer automating a local library, FreeBSD training lectures to schools, fixing BSD install etc for blind / half blind etc. Cheers, Julian -- Julian Stacey: BSDUnixLinux C Prog Admin SysEng Consult Munich www.berklix.com Mail plain ASCII text. HTML & Base64 text are spam. www.asciiribbon.org From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 16:30:58 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 51A131065672; Fri, 15 May 2009 16:30:58 +0000 (UTC) (envelope-from bright@elvis.mu.org) Received: from elvis.mu.org (elvis.mu.org [192.203.228.196]) by mx1.freebsd.org (Postfix) with ESMTP id 358448FC15; Fri, 15 May 2009 16:30:58 +0000 (UTC) (envelope-from bright@elvis.mu.org) Received: by elvis.mu.org (Postfix, from userid 1192) id 0AC2E1A3C3C; Fri, 15 May 2009 09:30:58 -0700 (PDT) Date: Fri, 15 May 2009 09:30:57 -0700 From: Alfred Perlstein To: hackers@freebsd.org Message-ID: <20090515163057.GB4062@elvis.mu.org> Mime-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <9740caf0905141119o193eda9h1bde4dbbb8f8645e@mail.gmail.com> User-Agent: Mutt/1.4.2.3i Cc: Matt Olander , Julian Stacey , Rayson Ho Subject: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 16:30:58 -0000 > On Thu, May 14, 2009 at 9:53 AM, Julian Stacey wrote: > > Hi hackers@ > > A commercial firm asked for _Free_ labour today on jobs at freebsd. > > The censors passed it. Censors of jobs at freebsd.org then blocked > > the posting below. jobs@ censors again bad, block wrong things, > > should all be removed & not replaced. > > > > Several suckers have already enquired to that firm. Hope we might get > > some Free labour to donate time to Freebsd, Not Stock holders ! > > Hi Julian, > > Internships are an accepted way for a high school or university > student (and nowadays some post grad students and others) to gain a > bit of experience in their field before joining the work force or > perhaps while switching careers. At my company, we've filled several > full-time positions with people that were interns first. It's just a > way to fill a part-time, sometimes non-paid job, at a company where > there isn't an official requisition for that particular position. > Nobody is forcing anybody to take the internship and it is clearly > stated that it is a non-paid internship in the post. > > I imagine that there would be some interested students or unemployed > people that would love to work with Alfred on a project at Juniper a > few hours a week in their spare time, for free. It will look great on > a resume, they will probably learn some valuable skills, and perhaps > parlay it into a full-time, paid position. > > best, > -matt Thanks Matt, this is my only intention. A few of the candidates I've spoken too are very excited to get something on their resume with a commercial entity and there is the hope that I may be able to hire one on them in the future. I've also promised the candidates that they will have access to some amazing resources within Juniper if (I can manage it) and at the very least I can mentor them on any FreeBSD endeavors they take on for the other non-2 hours per-day they would be working for me. While I would love to see more students working on FreeBSD, the fact of the matter is that some students already have worked on FreeBSD and would like commercial experience of "worked on a team in an office environment" that is challenging to mimic in our (FreeBSD's) distributed ways. At the end of the day, what FreeBSD-jobs is supposed to be is a place where jobs can be posted and found that will enable a FreeBSD fan to find suitable employment opportunities for a career, or to advance their career. The reason for moderation of FreeBSD-jobs is to prevent people such as Julian turning a well intentioned message into a thread of flames because he's gone imbalanced due to lack of coffee some morning. Effectively it's been a pretty swell system, FreeBSD-jobs has 0 spam (except to the poor moderators) and also insulated job seekers and posters from the typical hecklers who feel the need for extremely abusive emails due to some real or perceived mistake by the recruiter or job-seeker. I honestly feel that we've even saved plenty of people embarrassment by blocking or bouncing messages that they may have sent in haste to freebsd-jobs that after cooling off realized "the Internet is forever, why in g-d's name did I send something so mean with my name on it?!?". It's a shame it doesn't work for cross-list posts. I'm proud to be one of the moderators on FreeBSD-jobs, but I do admit most of the work is done by the other moderators. Thanks again Matt. I'm going to have to pick your brain later about how to deal with interns, care, feeding, hats? :) And Julian, chill out, I still cringe from embarrassment when someone drags out some old email _I_ sent with close to the same tone as the ones I've been seeing from you. Best of luck. -Alfred From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 16:48:20 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 8B004106564A for ; Fri, 15 May 2009 16:48:20 +0000 (UTC) (envelope-from ap@bnc.net) Received: from mailomat.net (mailomat.net [81.20.89.254]) by mx1.freebsd.org (Postfix) with ESMTP id 238558FC17 for ; Fri, 15 May 2009 16:48:19 +0000 (UTC) (envelope-from ap@bnc.net) X-Mailomat-SpamCatcher-Score: 2 [X] Received: from [194.39.192.125] (account bnc-mail@mailrelay.mailomat.net HELO bnc.net) by mailomat.net (CommuniGate Pro SMTP 5.2.8) with ESMTPSA id 49566737; Fri, 15 May 2009 17:48:17 +0200 X-Junk-Score: 2 [X] X-SpamCatcher-Score: 2 [X] Received: from [192.168.5.190] (account ap HELO [192.168.5.190]) by bnc.net (CommuniGate Pro SMTP 5.2.13) with ESMTPSA id 3441390; Fri, 15 May 2009 17:48:16 +0200 Message-Id: <790C89F7-2F10-4601-B984-64B3988BAF82@bnc.net> From: Achim Patzner To: "Julian Stacey" In-Reply-To: <200905151443.n4FEh9Tf027120@fire.js.berklix.net> Content-Type: text/plain; charset=US-ASCII; format=flowed Content-Transfer-Encoding: 7bit Mime-Version: 1.0 (Apple Message framework v935.3) Date: Fri, 15 May 2009 17:48:11 +0200 References: <200905151443.n4FEh9Tf027120@fire.js.berklix.net> X-Mailer: Apple Mail (2.935.3) Cc: hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 16:48:20 -0000 Am 15.05.2009 um 16:43 schrieb Julian Stacey: >> Internships are an accepted way for a high school or university > > In America. America imported unpaid apprenticeships & indentured > servitude (time limited slavery) from Europe/Britain centuries ago. Take this somewhere else, it's getting boring. Grown-ups should know what they're doing without your protection and the rest might learn a bit on their own. Achim Patzner From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 16:54:35 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 49865106564A for ; Fri, 15 May 2009 16:54:35 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from flat.berklix.org (flat.berklix.org [83.236.223.115]) by mx1.freebsd.org (Postfix) with ESMTP id C78F88FC19 for ; Fri, 15 May 2009 16:54:34 +0000 (UTC) (envelope-from jhs@berklix.org) Received: from js.berklix.net (p549A6C1C.dip.t-dialin.net [84.154.108.28]) (authenticated bits=0) by flat.berklix.org (8.13.8/8.13.8) with ESMTP id n4FGsSxL027677; Fri, 15 May 2009 18:54:29 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (fire.js.berklix.net [192.168.91.41]) by js.berklix.net (8.13.8/8.13.8) with ESMTP id n4FGsGju012838; Fri, 15 May 2009 18:54:16 +0200 (CEST) (envelope-from jhs@berklix.org) Received: from fire.js.berklix.net (localhost [127.0.0.1]) by fire.js.berklix.net (8.14.3/8.14.3) with ESMTP id n4FGsrLM028804; Fri, 15 May 2009 18:55:03 +0200 (CEST) (envelope-from jhs@fire.js.berklix.net) Message-Id: <200905151655.n4FGsrLM028804@fire.js.berklix.net> To: Achim Patzner From: "Julian Stacey" Organization: http://berklix.com BSD Unix Linux Consultancy, Munich Germany User-agent: EXMH on FreeBSD http://berklix.com/free/ X-URL: http://berklix.com In-reply-to: Your message "Fri, 15 May 2009 17:48:11 +0200." <790C89F7-2F10-4601-B984-64B3988BAF82@bnc.net> Date: Fri, 15 May 2009 18:54:53 +0200 Sender: jhs@berklix.org Cc: hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 16:54:35 -0000 > >> Internships are an accepted way for a high school or university > > > > In America. America imported unpaid apprenticeships & indentured > > servitude (time limited slavery) from Europe/Britain centuries ago. > > Take this somewhere else, it's getting boring. Grown-ups should know > what they're doing without your protection and the rest might learn > a bit on their own. You'r right on adults & free choice, I'll drop that rather than drift. What I was trying to illustrate is what jobs@ censors pass & block. - jobs@ is censored, so jobs@ censors performance cant be discussed on jobs@. - Those that pushed to censor jobs@ some years ago (& succesors?) are not worth having, jobs@FreeBSD would be better without them. - Censors of jobs@ do not have the courage to announce on footer or header of jobs@ that they censor jobs@freebsd. - Most don't know jobs@freebsd Is censored. Most think only announce@ is moderated , & maybe arch@. - Moving to chat@ is for things that drift off from FreeSBD, but FreeBSD censorship Is relevant to FreeBSD, - Where better than hackers@ to look for support to liberate jobs@freebsd from censors ? Cheers, Julian -- Julian Stacey: BSDUnixLinux C Prog Admin SysEng Consult Munich www.berklix.com Mail plain ASCII text. HTML & Base64 text are spam. www.asciiribbon.org From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 17:43:28 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 7E7591065670 for ; Fri, 15 May 2009 17:43:28 +0000 (UTC) (envelope-from xcllnt@mac.com) Received: from asmtpout013.mac.com (asmtpout013.mac.com [17.148.16.88]) by mx1.freebsd.org (Postfix) with ESMTP id 6B08B8FC15 for ; Fri, 15 May 2009 17:43:28 +0000 (UTC) (envelope-from xcllnt@mac.com) MIME-version: 1.0 Content-transfer-encoding: 7BIT Content-type: text/plain; charset=US-ASCII; format=flowed; delsp=yes Received: from mly-t60.jnpr.net (natint3.juniper.net [66.129.224.36]) by asmtp013.mac.com (Sun Java(tm) System Messaging Server 6.3-8.01 (built Dec 16 2008; 32bit)) with ESMTPSA id <0KJP00HKL2F9HM00@asmtp013.mac.com> for hackers@freebsd.org; Fri, 15 May 2009 09:42:46 -0700 (PDT) Message-id: <70A19896-8F17-4D20-998B-CE6644B1E969@mac.com> From: Marcel Moolenaar To: Julian Stacey In-reply-to: <200905151443.n4FEh9Tf027120@fire.js.berklix.net> Date: Fri, 15 May 2009 09:42:44 -0700 References: <200905151443.n4FEh9Tf027120@fire.js.berklix.net> X-Mailer: Apple Mail (2.935.3) Cc: matt@ixsystems.com, hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 17:43:29 -0000 On May 15, 2009, at 7:43 AM, Julian Stacey wrote: > Hi Matt, >>> Several suckers have already enquired to that firm. =A0Hope we >>> might get >>> some Free labour to donate time to Freebsd, Not Stock holders ! >> >> Hi Julian, >> Internships are an accepted way for a high school or university > > In America. America imported unpaid apprenticeships & indentured > servitude (time limited slavery) from Europe/Britain centuries ago. > Britain dumped both Long since. (Germany still has some interns > eg in theatre, last described as a rip off). Condolences that the > "Land of the free" retains medieval European intern practice. *plonk* -- Marcel Moolenaar xcllnt@mac.com From owner-freebsd-hackers@FreeBSD.ORG Fri May 15 17:29:16 2009 Return-Path: Delivered-To: hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id BCBE21065670 for ; Fri, 15 May 2009 17:29:16 +0000 (UTC) (envelope-from linimon@lonesome.com) Received: from mail.soaustin.net (lefty.soaustin.net [66.135.55.46]) by mx1.freebsd.org (Postfix) with ESMTP id 9E2AE8FC1A for ; Fri, 15 May 2009 17:29:16 +0000 (UTC) (envelope-from linimon@lonesome.com) Received: by mail.soaustin.net (Postfix, from userid 502) id 2EFFA8C049; Fri, 15 May 2009 12:10:02 -0500 (CDT) Date: Fri, 15 May 2009 12:10:02 -0500 From: Mark Linimon To: Julian Stacey Message-ID: <20090515171002.GA24620@lonesome.com> References: <790C89F7-2F10-4601-B984-64B3988BAF82@bnc.net> <200905151655.n4FGsrLM028804@fire.js.berklix.net> MIME-Version: 1.0 Content-Type: text/plain; charset=us-ascii Content-Disposition: inline In-Reply-To: <200905151655.n4FGsrLM028804@fire.js.berklix.net> User-Agent: Mutt/1.5.18 (2008-05-17) X-Mailman-Approved-At: Fri, 15 May 2009 17:52:54 +0000 Cc: Achim Patzner , hackers@freebsd.org Subject: Re: FreeBSD jobs X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 May 2009 17:29:17 -0000 On Fri, May 15, 2009 at 06:54:53PM +0200, Julian Stacey wrote: > - Those that pushed to censor jobs@ some years ago (& succesors?) > are not worth having, jobs@FreeBSD would be better without them. In your opinion. Not in mine. > - Where better than hackers@ to look for support to liberate > jobs@freebsd from censors ? chat@. mcl From owner-freebsd-hackers@FreeBSD.ORG Sat May 16 09:37:18 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id AEACE106566B for ; Sat, 16 May 2009 09:37:18 +0000 (UTC) (envelope-from stas@FreeBSD.org) Received: from mx0.deglitch.com (backbone.deglitch.com [IPv6:2001:16d8:fffb:4::abba]) by mx1.freebsd.org (Postfix) with ESMTP id 6089F8FC16 for ; Sat, 16 May 2009 09:37:18 +0000 (UTC) (envelope-from stas@FreeBSD.org) Received: from DSPAM-Daemon (localhost [127.0.0.1]) by mx0.deglitch.com (Postfix) with SMTP id 515AD8FC1D for ; Sat, 16 May 2009 13:37:16 +0400 (MSD) Received: from orion.SpringDaemons.com (unknown [77.232.3.143]) by mx0.deglitch.com (Postfix) with ESMTPA id C4DF38FC18; Sat, 16 May 2009 13:37:15 +0400 (MSD) Received: from orion (localhost [127.0.0.1]) by orion.SpringDaemons.com (Postfix) with SMTP id 45C863982B; Sat, 16 May 2009 13:37:47 +0400 (MSD) Date: Sat, 16 May 2009 13:37:42 +0400 From: Stanislav Sedov To: =?KOI8-R?Q?=EF=CC=C5=C7_=F0=C5=D4=D2=C1=DE=A3=D7?= Message-Id: <20090516133742.0e26a347.stas@FreeBSD.org> In-Reply-To: <4A0C0187.1030107@sprinthost.ru> References: <4A0C0187.1030107@sprinthost.ru> Organization: The FreeBSD Project X-XMPP: ssedov@jabber.ru X-Voice: +7 916 849 20 23 X-PGP-Fingerprint: F21E D6CC 5626 9609 6CE2 A385 2BF5 5993 EB26 9581 X-Mailer: carrier-pigeon Mime-Version: 1.0 Content-Type: text/plain; charset=KOI8-R Content-Transfer-Encoding: 8bit X-DSPAM-Result: Innocent X-DSPAM-Processed: Sat May 16 13:37:16 2009 X-DSPAM-Confidence: 0.9899 X-DSPAM-Improbability: 1 in 9809 chance of being spam X-DSPAM-Probability: 0.0000 X-DSPAM-Signature: 4a0e894c994291748722663 Cc: freebsd-hackers@freebsd.org Subject: Re: ipfw uid rules for lo0 interface X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 16 May 2009 09:37:18 -0000 -----BEGIN PGP SIGNED MESSAGE----- Hash: SHA1 On Thu, 14 May 2009 15:33:27 +0400 ïÌÅÇ ðÅÔÒÁÞ£× mentioned: > Hello! > > I am using FreeBSD 7.2-RELEASE. > > I am trying to restrict connections to local smtp daemon to limited > number of users. But when I create rules for ipfw with uid pattern, I > don't get the desired result: all connections on 25 port are blocked and > it is impossible to allow it for anyone. > > I am using the following rules (let's say only root is allowed send > messages): > > # ipfw flush > # ipfw add 100 allow ip from any to me 25 uid root > # ipfw add 200 deny ip from any to me 25 > > # telnet localhost 25 > Trying 127.0.0.1... > > And nothing is happening - the connection is neither allowed nor denied, > it just hangs. > > What am I doing wrong? Thanks in advance! > That should work. I suspect you don't have anything running on 127.0.0.1:25, otherwise you should have been receiving a "permission denied" message. You can inspect what's binded on which ports/addresses by running `sockstat -4`. - -- Stanislav Sedov ST4096-RIPE -----BEGIN PGP SIGNATURE----- iEYEARECAAYFAkoOiWsACgkQK/VZk+smlYFcpACeMLylEJRGrP7w0ciiHqT+Xhzz QEsAn2AU5chm06vYZBrX8/7mSDfpnD8P =blL4 -----END PGP SIGNATURE----- !DSPAM:4a0e894c994291748722663! From owner-freebsd-hackers@FreeBSD.ORG Sat May 16 17:05:29 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id CEDDE106564A for ; Sat, 16 May 2009 17:05:29 +0000 (UTC) (envelope-from to.my.trociny@gmail.com) Received: from fg-out-1718.google.com (fg-out-1718.google.com [72.14.220.152]) by mx1.freebsd.org (Postfix) with ESMTP id 514808FC08 for ; Sat, 16 May 2009 17:05:28 +0000 (UTC) (envelope-from to.my.trociny@gmail.com) Received: by fg-out-1718.google.com with SMTP id e12so286777fga.12 for ; Sat, 16 May 2009 10:05:28 -0700 (PDT) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/relaxed; d=gmail.com; s=gamma; h=domainkey-signature:received:received:to:cc:subject:references :organization:from:date:in-reply-to:message-id:user-agent :mime-version:content-type:content-transfer-encoding; bh=2+ZSjQJ642MIJkB8TDQWnWcV3KEZQhk8jf+XO9/qv/E=; b=akXst155L618Mjn6LXbgZvRblCke0MMz+Y4eyweailwurXszSJFeEhvqwGFFnXKqpn dEJUZ6QbgJHXerxD6p5IbIiYtJ7N9NEGunlX73JT/TPXnmGWb9EDJOBVov2DlndDsJf8 iLZDNN5oWzfxeaDi0zXfMedZGfi4lTSpg5n9A= DomainKey-Signature: a=rsa-sha1; c=nofws; d=gmail.com; s=gamma; h=to:cc:subject:references:organization:from:date:in-reply-to :message-id:user-agent:mime-version:content-type :content-transfer-encoding; b=AEsdPf+yWxfYXA0UcYA4f8vfPb3mE1V0CIkf888sM5/ojAxeW511lc5bLKLyGbN/j5 dFDkwNTUTskMdlBYhmGXXzl5RC6XI4NqZewXIzIUiHNSsaW/zZeiFEgEC1kUX1zhUIrE /kZYKrKvUpH2oeui5hjBU1FSguimdxXSvPkYc= Received: by 10.86.68.10 with SMTP id q10mr4973012fga.78.1242493528172; Sat, 16 May 2009 10:05:28 -0700 (PDT) Received: from localhost ([95.69.165.249]) by mx.google.com with ESMTPS id d6sm4610917fga.2.2009.05.16.10.05.25 (version=TLSv1/SSLv3 cipher=RC4-MD5); Sat, 16 May 2009 10:05:26 -0700 (PDT) To: Marius =?iso-8859-1?Q?N=FCnnerich?= References: <814ovqn8dp.fsf@zhuzha.ua1> Organization: TOA Ukraine From: Mikolaj Golub Date: Sat, 16 May 2009 20:05:24 +0300 In-Reply-To: ("Marius =?iso-8859-1?Q?N=FCnnerich=22's?= message of "Fri\, 15 May 2009 13\:48\:51 +0200") Message-ID: <86k54hvuzv.fsf@kopusha.onet> User-Agent: Gnus/5.11 (Gnus v5.11) Emacs/22.1 (berkeley-unix) MIME-Version: 1.0 Content-Type: text/plain; charset=iso-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org, Mikolaj Golub Subject: Re: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 16 May 2009 17:05:30 -0000 On Fri, 15 May 2009 13:48:51 +0200 Marius N=FCnnerich wrote: MN> On Tue, May 12, 2009 at 08:27, Mikolaj Golub = wrote: >> Hi, >> >> The code below is compiled with -fopenmp and run on FreeBSD6/7 (i386, a= md64): >> >> #include >> #include >> >> int n =3D 4, m =3D 2; >> >> int main () { >> =A0 =A0 =A0 =A0for (;;) { >> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0int i; >> >> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); >> #pragma omp parallel for num_threads(m) >> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} >> >> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); >> #pragma omp parallel for num_threads(n) >> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} >> >> =A0 =A0 =A0 =A0} >> >> =A0 =A0 =A0 =A0return 0; >> } >> >> During the run the program's virtual memory usage constantly grows. The= growth >> is observed only when n !=3D m. When running the program with uncomment= ed >> sleep() and observing the number of threads with 'top -H' I see in turn= 2 or 4 >> threads. So it looks like memory leak when thread is removed. Should I = fill >> PR? It looks like I have found the leak. The problem is in libgomp/team.c. gomp_thread_start() does sem_init() but sem_destroy() is never called. This patch solves the problem for me: --- contrib/gcclibs/libgomp/team.c.orig 2009-05-16 17:32:57.000000000 +0300 +++ contrib/gcclibs/libgomp/team.c 2009-05-16 19:16:37.000000000 +0300 @@ -164,9 +164,12 @@ new_team (unsigned nthreads, struct gomp static void free_team (struct gomp_team *team) { + int i; free (team->work_shares); gomp_mutex_destroy (&team->work_share_lock); gomp_barrier_destroy (&team->barrier); + for(i =3D 1; i < team->nthreads; i++) + gomp_sem_destroy (team->ordered_release[i]); gomp_sem_destroy (&team->master_release); free (team); } I am going to fill PR to gcc mainstream, but should I also register this in FreeBSD bugtrack as gcc is part of the base? BTW, the problem is not observed under Linux. I have not looked in Linux co= de but it looks like sem_init() implementation for Linux does not do memory allocation. The memory for the test program below grows under FreeBSD and d= oes not under Linux. #include int main(int argc, char *argv[]) { sem_t sem; for(;;) { sem_init(&sem, 0, 0);} return 0; } MN> I can confirm this. I briefly looked through the libgomp code but MN> didn't see the leak. Anybody knows good tools how to investigate this? http://freshmeat.net/projects/lmdbg This is a small memory leak debugger. It does not provide all functionality you can find in more sophisticated tools but is lightweight, portable and simple in use. It was very useful when I traced this bug. --=20 Mikolaj Golub From owner-freebsd-hackers@FreeBSD.ORG Sat May 16 18:22:17 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id 741D4106564A for ; Sat, 16 May 2009 18:22:17 +0000 (UTC) (envelope-from pieter@degoeje.nl) Received: from mx.utwente.nl (mx3.utsp.utwente.nl [130.89.2.14]) by mx1.freebsd.org (Postfix) with ESMTP id E9EC48FC1B for ; Sat, 16 May 2009 18:22:16 +0000 (UTC) (envelope-from pieter@degoeje.nl) Received: from nox.student.utwente.nl (nox.student.utwente.nl [130.89.165.91]) by mx.utwente.nl (8.12.10/SuSE Linux 0.7) with ESMTP id n4GILkkk002602; Sat, 16 May 2009 20:21:46 +0200 From: Pieter de Goeje To: freebsd-hackers@freebsd.org Date: Sat, 16 May 2009 20:21:32 +0000 User-Agent: KMail/1.11.3 (FreeBSD/8.0-CURRENT; KDE/4.2.3; amd64; ; ) References: <814ovqn8dp.fsf@zhuzha.ua1> <86k54hvuzv.fsf@kopusha.onet> In-Reply-To: <86k54hvuzv.fsf@kopusha.onet> MIME-Version: 1.0 Content-Type: Text/Plain; charset="iso-8859-1" Content-Transfer-Encoding: quoted-printable Content-Disposition: inline Message-Id: <200905162021.32545.pieter@degoeje.nl> X-UTwente-MailScanner-Information: Scanned by MailScanner. Contact servicedesk@icts.utwente.nl for more information. X-UTwente-MailScanner: Found to be clean X-UTwente-MailScanner-SpamScore: s X-UTwente-MailScanner-From: pieter@degoeje.nl X-Spam-Status: No Cc: =?iso-8859-1?q?N=FCnnerich?= , Mikolaj Golub , Marius Subject: Re: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 16 May 2009 18:22:17 -0000 On Saturday 16 May 2009 17:05:24 Mikolaj Golub wrote: > On Fri, 15 May 2009 13:48:51 +0200 Marius N=FCnnerich wrote: > > MN> On Tue, May 12, 2009 at 08:27, Mikolaj Golub =20 wrote: > >> Hi, > >> > >> The code below is compiled with -fopenmp and run on FreeBSD6/7 (i386, > >> amd64): > >> > >> #include > >> #include > >> > >> int n =3D 4, m =3D 2; > >> > >> int main () { > >> for (;;) { > >> int i; > >> > >> //sleep(2); > >> #pragma omp parallel for num_threads(m) > >> for(i =3D 0; i < 1; i++) {} > >> > >> //sleep(2); > >> #pragma omp parallel for num_threads(n) > >> for(i =3D 0; i < 1; i++) {} > >> > >> } > >> > >> return 0; > >> } > >> > >> During the run the program's virtual memory usage constantly grows. T= he > >> growth is observed only when n !=3D m. When running the program with > >> uncommented sleep() and observing the number of threads with 'top -H'= I > >> see in turn 2 or 4 threads. So it looks like memory leak when thread = is > >> removed. Should I fill PR? > > It looks like I have found the leak. The problem is in libgomp/team.c. > gomp_thread_start() does sem_init() but sem_destroy() is never called. Th= is > patch solves the problem for me: > > --- contrib/gcclibs/libgomp/team.c.orig 2009-05-16 17:32:57.000000000 +03= 00 > +++ contrib/gcclibs/libgomp/team.c 2009-05-16 19:16:37.000000000 +03= 00 > @@ -164,9 +164,12 @@ new_team (unsigned nthreads, struct gomp > static void > free_team (struct gomp_team *team) > { > + int i; > free (team->work_shares); > gomp_mutex_destroy (&team->work_share_lock); > gomp_barrier_destroy (&team->barrier); > + for(i =3D 1; i < team->nthreads; i++) > + gomp_sem_destroy (team->ordered_release[i]); > gomp_sem_destroy (&team->master_release); > free (team); > } > > I am going to fill PR to gcc mainstream, but should I also register this = in > FreeBSD bugtrack as gcc is part of the base? > > BTW, the problem is not observed under Linux. I have not looked in Linux > code but it looks like sem_init() implementation for Linux does not do > memory allocation. The memory for the test program below grows under > FreeBSD and does not under Linux. Note that libgomp uses it's own implementation of POSIX semaphores (using=20 phtread mutexes) instead of FreeBSD's sem(4). If the program below is run=20 against FreeBSD's implementation, it quickly stops growing because there is= a=20 limit on the number of allocated semaphores. It would be interesting to see if there are any differences performance wis= e=20 between the two. If the native version is faster, it might be another reaso= n=20 to include sem(4) in the GENERIC kernel... > > #include > > int > main(int argc, char *argv[]) { > > sem_t sem; > > for(;;) { sem_init(&sem, 0, 0);} > > return 0; > } =2D- Pieter de Goeje From owner-freebsd-hackers@FreeBSD.ORG Sat May 16 18:24:10 2009 Return-Path: Delivered-To: freebsd-hackers@freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:4f8:fff6::34]) by hub.freebsd.org (Postfix) with ESMTP id B9DEC1065679 for ; Sat, 16 May 2009 18:24:10 +0000 (UTC) (envelope-from marius@nuenneri.ch) Received: from yw-out-2324.google.com (yw-out-2324.google.com [74.125.46.29]) by mx1.freebsd.org (Postfix) with ESMTP id 7D7748FC1E for ; Sat, 16 May 2009 18:24:10 +0000 (UTC) (envelope-from marius@nuenneri.ch) Received: by yw-out-2324.google.com with SMTP id 9so1473721ywe.13 for ; Sat, 16 May 2009 11:24:09 -0700 (PDT) MIME-Version: 1.0 Received: by 10.151.73.9 with SMTP id a9mr8625863ybl.60.1242498249855; Sat, 16 May 2009 11:24:09 -0700 (PDT) In-Reply-To: <86k54hvuzv.fsf@kopusha.onet> References: <814ovqn8dp.fsf@zhuzha.ua1> <86k54hvuzv.fsf@kopusha.onet> Date: Sat, 16 May 2009 20:24:09 +0200 Message-ID: From: =?ISO-8859-1?Q?Marius_N=FCnnerich?= To: Mikolaj Golub Content-Type: text/plain; charset=ISO-8859-1 Content-Transfer-Encoding: quoted-printable Cc: freebsd-hackers@freebsd.org Subject: Re: Memory leak on thread removal X-BeenThere: freebsd-hackers@freebsd.org X-Mailman-Version: 2.1.5 Precedence: list List-Id: Technical Discussions relating to FreeBSD List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Sat, 16 May 2009 18:24:11 -0000 On Sat, May 16, 2009 at 19:05, Mikolaj Golub wrot= e: > > On Fri, 15 May 2009 13:48:51 +0200 Marius N=FCnnerich wrote: > > =A0MN> On Tue, May 12, 2009 at 08:27, Mikolaj Golub wrote: > =A0>> Hi, > =A0>> > =A0>> The code below is compiled with -fopenmp and run on FreeBSD6/7 (i38= 6, amd64): > =A0>> > =A0>> #include > =A0>> #include > =A0>> > =A0>> int n =3D 4, m =3D 2; > =A0>> > =A0>> int main () { > =A0>> =A0 =A0 =A0 =A0for (;;) { > =A0>> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0int i; > =A0>> > =A0>> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); > =A0>> #pragma omp parallel for num_threads(m) > =A0>> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} > =A0>> > =A0>> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0//sleep(2); > =A0>> #pragma omp parallel for num_threads(n) > =A0>> =A0 =A0 =A0 =A0 =A0 =A0 =A0 =A0for(i =3D 0; i < 1; i++) {} > =A0>> > =A0>> =A0 =A0 =A0 =A0} > =A0>> > =A0>> =A0 =A0 =A0 =A0return 0; > =A0>> } > =A0>> > =A0>> During the run the program's virtual memory usage constantly grows.= The growth > =A0>> is observed only when n !=3D m. When running the program with uncom= mented > =A0>> sleep() and observing the number of threads with 'top -H' I see in = turn 2 or 4 > =A0>> threads. So it looks like memory leak when thread is removed. Shoul= d I fill > =A0>> PR? > > It looks like I have found the leak. The problem is in libgomp/team.c. > gomp_thread_start() does sem_init() but sem_destroy() is never called. Th= is > patch solves the problem for me: > > --- contrib/gcclibs/libgomp/team.c.orig 2009-05-16 17:32:57.000000000 +03= 00 > +++ contrib/gcclibs/libgomp/team.c =A0 =A0 =A02009-05-16 19:16:37.0000000= 00 +0300 > @@ -164,9 +164,12 @@ new_team (unsigned nthreads, struct gomp > =A0static void > =A0free_team (struct gomp_team *team) > =A0{ > + =A0int i; > =A0 free (team->work_shares); > =A0 gomp_mutex_destroy (&team->work_share_lock); > =A0 gomp_barrier_destroy (&team->barrier); > + =A0for(i =3D 1; i < team->nthreads; i++) > + =A0 =A0gomp_sem_destroy (team->ordered_release[i]); > =A0 gomp_sem_destroy (&team->master_release); > =A0 free (team); > =A0} > > I am going to fill PR to gcc mainstream, but should I also register this = in > FreeBSD bugtrack as gcc is part of the base? > > BTW, the problem is not observed under Linux. I have not looked in Linux = code > but it looks like sem_init() implementation for Linux does not do memory > allocation. The memory for the test program below grows under FreeBSD and= does > not under Linux. > > #include > > int > main(int argc, char *argv[]) { > > =A0 =A0 =A0 =A0sem_t sem; > > =A0 =A0 =A0 =A0for(;;) { sem_init(&sem, 0, 0);} > > =A0 =A0 =A0 =A0return 0; > } Wow! Thanks for tracking this down. I think you can file both PR's so that FreeBSD can include your patch before it comes in via upstream. > > > =A0MN> I can confirm this. I briefly looked through the libgomp code but > =A0MN> didn't see the leak. Anybody knows good tools how to investigate t= his? > > http://freshmeat.net/projects/lmdbg > > This is a small memory leak debugger. It does not provide all functionali= ty > you can find in more sophisticated tools but is lightweight, portable and > simple in use. It was very useful when I traced this bug. Thanks, I'll take a look at it.