NetBSD Problem Report #55889

From www@netbsd.org  Mon Dec 21 17:10:03 2020
Return-Path: <www@netbsd.org>
Received: from mail.netbsd.org (mail.netbsd.org [199.233.217.200])
	(using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits))
	(Client CN "mail.NetBSD.org", Issuer "mail.NetBSD.org CA" (not verified))
	by mollari.NetBSD.org (Postfix) with ESMTPS id 691681A921F
	for <gnats-bugs@gnats.NetBSD.org>; Mon, 21 Dec 2020 17:10:03 +0000 (UTC)
Message-Id: <20201221171002.151951A9239@mollari.NetBSD.org>
Date: Mon, 21 Dec 2020 17:10:02 +0000 (UTC)
From: hashikaw@mail.ru
Reply-To: hashikaw@mail.ru
To: gnats-bugs@NetBSD.org
Subject: panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware)
X-Send-Pr-Version: www-1.0

>Number:         55889
>Category:       kern
>Synopsis:       panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware)
>Confidential:   no
>Severity:       critical
>Priority:       medium
>Responsible:    kern-bug-people
>State:          closed
>Class:          sw-bug
>Submitter-Id:   net
>Arrival-Date:   Mon Dec 21 17:15:01 +0000 2020
>Closed-Date:    Sat Apr 03 07:28:49 +0000 2021
>Last-Modified:  Sat Apr 03 07:28:49 +0000 2021
>Originator:     Kouichi Hashikawa
>Release:        NetBSD-9.99.77
>Organization:
>Environment:
NetBSD 9.99.77 (GENERIC64) #0: Mon Dec 21 02:38:57 UTC 2020
 	mkrepro@mkrepro.NetBSD.org:/usr/src/sys/arch/evbarm/compile/GENERIC64
>Description:
when use -current kernel on RPi4 and without RPi4_UEFI_Firmware,
panic with message,

[   1.5130955] panic: kernel diagnostic assertion "l->l_stat == LSONPROC" failed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227 
[   1.5230984] cpu2: Begin traceback...
[   1.5230984] trace fp ffffc00060f1f9e0
[   1.5330967] fp ffffc00060f1fa10 vpanic() at ffffc000004e59b4 netbsd:vpanic+0x14c
[   1.5330967] fp ffffc00060f1fa70 kern_assert() at ffffc0000080bc7c netbsd:kern_assert+0x5c
[   1.5430982] fp ffffc00060f1fb00 sleepq_enqueue() at ffffc000004b14e0 netbsd:sleepq_enqueue+0x108
[   1.5530977] fp ffffc00060f1fb40 cv_wait() at ffffc00000478818 netbsd:cv_wait+0xe8
[   1.5630988] fp ffffc00060f1fb80 xc_wait() at ffffc000004ef920 netbsd:xc_wait+0xb0
[   1.5730988] fp ffffc00060f1fbc0 percpu_backend_alloc() at ffffc000004dd6c8 netbsd:percpu_backend_alloc+0x150
[   1.5830999] fp ffffc00060f1fc40 vmem_xalloc() at ffffc000004ed2cc netbsd:vmem_xalloc+0x6ac
[   1.5830999] fp ffffc00060f1fd20 vmem_alloc() at ffffc000004ed704 netbsd:vmem_alloc+0x84
[   1.5930999] fp ffffc00060f1fd80 percpu_create() at ffffc000004dde5c netbsd:percpu_create+0x3c
[   1.6031014] fp ffffc00060f1fe00 pic_add() at ffffc00000003114 netbsd:pic_add+0xfc
[   1.6131010] fp ffffc00060f1fe40 bcm2836mp_intr_init() at ffffc00000018170 netbsd:bcm2836mp_intr_init+0x90
[   1.6231027] fp ffffc00060f1fe90 arm_fdt_cpu_hatch() at ffffc000000641c8 netbsd:arm_fdt_cpu_hatch+0x28
[   1.6331021] fp ffffc00060f1feb0 cpu_hatch() at ffffc00000084064 netbsd:cpu_hatch+0x8c
[   1.6431032] fp 0000000000000000 cpu_mpstart() at ffffc00000001a84 netbsd:cpu_mpstart+0x19c
[   1.6431032] cpu2: End traceback...
Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4:        ret


-current kernel can boot with RPi4_UEFI_Firmware.
>How-To-Repeat:

>Fix:

>Release-Note:

>Audit-Trail:
From: mlelstv@serpens.de (Michael van Elst)
To: gnats-bugs@netbsd.org
Cc: 
Subject: Re: kern/55889: panic when boot GENERIC64 kernel on RaspberryPi4 (without RPi4_UEFI_Firmware)
Date: Mon, 21 Dec 2020 18:00:13 -0000 (UTC)

 hashikaw@mail.ru writes:

 >when use -current kernel on RPi4 and without RPi4_UEFI_Firmware,
 >panic with message,

 >[   1.5130955] panic: kernel diagnostic assertion "l->l_stat == LSONPROC" failed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227 

 The percpu allocation needs to synchronize with other CPUs and this
 fails because the process isn't correctly initialized as LSONPROC yet.


 >[   1.6131010] fp ffffc00060f1fe40 bcm2836mp_intr_init() at ffffc00000018170 netbsd:bcm2836mp_intr_init+0x90

 A crude workaround is to skip bcm2836mp_intr_init() for aarch64.

 --- bcm2835_intr.c      16 Dec 2020 19:49:04 -0000      1.33
 +++ bcm2835_intr.c      21 Dec 2020 17:58:48 -0000
 @@ -313,7 +358,9 @@ bcm2835_icu_attach(device_t parent, devi
                 ifuncs = &bcm2836mpicu_fdt_funcs;

                 bcm2836mp_intr_init(self, curcpu());
 +#ifndef __aarch64__
                 arm_fdt_cpu_hatch_register(self, bcm2836mp_intr_init);
 +#endif
         } else {
                 if (bcml1icu_sc == NULL)
                         arm_fdt_irq_set_handler(bcm2835_irq_handler);

 -- 
 -- 
                                 Michael van Elst
 Internet: mlelstv@serpens.de
                                 "A potential Snark may lurk in every tree."

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: mlelstv@serpens.de
Subject: Re: kern/55889: panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware)
Date: Tue, 22 Dec 2020 19:42:36 +0900

 > A crude workaround is to skip bcm2836mp_intr_init() for aarch64.

 -current kernel can boot with your patch. Thank you.

 > The percpu allocation needs to synchronize with other CPUs and this fails b=
 ecause the process isn't correctly initialized as LSONPROC yet.

 I add aprint_normal() at l->l_stat =3D LSONPROC in kern_synch.c, kern_softin=
 t.c,
 kern_sleepq.c, kern_lwp.c and make kernel and boot several times.
 Panic occured after kern_softint.c:softint_dispatch().

 I add KASSERT(1=3D=3D0) at softint_dispatch(), I got following trace.


 [   1.4669126] panic: kernel diagnostic assertion "1=3D=3D0" failed: file "/=
 curren
 t/netbsd/c/src/sys/kern/kern_softint.c", line 803=20
 [   1.4669126] cpu0: Begin traceback...
 [   1.4669126] trace fp ffffc00060e6fbd0
 [   1.4669126] fp ffffc00060e6fc00 vpanic() at ffffc000004e59cc netbsd:vpani=
 c+
 0x14c
 [   1.4669126] fp ffffc00060e6fc60 kern_assert() at ffffc0000080bc7c netbsd:=
 ke
 rn_assert+0x5c
 [   1.4669126] fp ffffc00060e6fd30 softint_dispatch() at ffffc000004b26d8 ne=
 tb
 sd:softint_dispatch+0x88
 [   1.4669126] fp ffffc000011b2a90 cpu_switchto_softint() at ffffc0000008c71=
 8=20
 netbsd:cpu_switchto_softint+0x6c
 [   1.4669126] tf ffffc000011b2ae0 el1_trap() at ffffc00000092f84 netbsd:el1=
 _t
 rap
 [   1.4669126] ---- trapframe 0xffffc000011b2ae0 (304 bytes) ----
 [   1.4669126]     pc=3Dffffc00000087674,   spsr=3D0000000000000005
 [   1.4669126]    esr=3D0000000000000000,    far=3D0000000000000000
 [   1.4669126]     x0=3D000000000000000e,     x1=3D000000000000000e
 [   1.4669126]     x2=3D0000000000000000,     x3=3D0000000000000000
 [   1.4669126]     x4=3Dffffc00001195998,     x5=3Dffffc00000e2e980
 [   1.4669126]     x6=3D0000000000000000,     x7=3D0000000000000007
 [   1.4669126]     x8=3Dffffc000011b2e20,     x9=3D00000000ffffffc8
 [   1.4669126]    x10=3Dffffc00000bd4e58,    x11=3D000000000000003f
 [   1.4669126]    x12=3Dfffffc0003ebbbe8,    x13=3Dfffffc0003ebbbed
 [   1.4669126]    x14=3D0000000044ca02be,    x15=3Dffffc000011b2e50
 [   1.4669126]    x16=3Dffffc000008001e8,    x17=3Dffffc00000b4a768
 [   1.4669126]    x18=3D000000000000000f,    x19=3D0000000000000000
 [   1.4669126]    x20=3D0000000000000001,    x21=3Dffffc00001195980
 [   1.4669126]    x22=3Dffffc00001195900,    x23=3Dffffc000011a9e90
 [   1.4669126]    x24=3D0000000000000001,    x25=3Dffffc000011a9000
 [   1.4669126]    x26=3D0000000000000002,    x27=3D0000000000000050
 [   1.4669126]    x28=3D000000003297c000, fp=3Dx29=3Dffffc000011b2e10
 [   1.4669126] lr=3Dx30=3Dffffc00000087678,     sp=3Dffffc000011b2e10
 [   1.4669126] ------------------------------------------------
 [   1.4669126] fp ffffc000011b2e10 cpu_boot_secondary_processors() at ffffc0=
 00
 00087674 netbsd:cpu_boot_secondary_processors+0xe4
 [   1.4669126] fp ffffc000011b2e60 main() at ffffc0000080bfe8 netbsd:main+0x=
 36
 8
 [   1.4669126] fp 0000000000000000 aarch64_start() at ffffc0000000187c netbs=
 d:
 aarch64_start+0x107c
 [   1.4669126] cpu0: End traceback...
 Stopped in pid 0.5 (system) at  netbsd:cpu_Debugger+0x4:        ret
 db{0}>=

State-Changed-From-To: open->feedback
State-Changed-By: skrll@NetBSD.org
State-Changed-When: Sat, 20 Feb 2021 21:12:46 +0000
State-Changed-Why:
This should be fixed in HEAD. Please update and report back.


From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: skrll@netbsd.org
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Sun, 21 Feb 2021 21:55:59 +0900

 --Apple-Mail-3632CC7C-C285-4D44-AA8A-07E7A1A0178A
 Content-Type: text/plain;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 =EF=BB=BF
 =EF=BB=BF
 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.=20

 I tried following image, but still panic.
 http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/202102202230Z/evbarm-aarch64/b=
 inary/gzimg/arm64mbr.img.gz



 [   1.0000030] entropy: WARNING: extracting entropy too early
 [   1.4100223] panic: kernel diagnostic assertion "l->l_stat =3D=3D LSONPROC=
 " fail
 ed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227=20
 [   1.4200249] cpu2: Begin traceback...
 [   1.4200249] trace fp ffffc00060ddf9e0
 [   1.4300234] fp ffffc00060ddfa10 vpanic() at ffffc0000050952c netbsd:vpani=
 c+
 0x14c
 [   1.4300234] fp ffffc00060ddfa70 kern_assert() at ffffc0000075bbbc netbsd:=
 ke
 rn_assert+0x5c
 [   1.4400250] fp ffffc00060ddfb00 sleepq_enqueue() at ffffc000004d4908 netb=
 sd
 :sleepq_enqueue+0x108
 [   1.4500245] fp ffffc00060ddfb40 cv_wait() at ffffc0000049ba88 netbsd:cv_w=
 ai
 t+0xe8
 [   1.4600255] fp ffffc00060ddfb80 xc_wait() at ffffc00000513498 netbsd:xc_w=
 ai
 t+0xb0
 [   1.4700256] fp ffffc00060ddfbc0 percpu_backend_alloc() at ffffc0000050124=
 0=20
 netbsd:percpu_backend_alloc+0x150
 [   1.4800319] fp ffffc00060ddfc40 vmem_xalloc() at ffffc00000510e44 netbsd:=
 vm
 em_xalloc+0x6ac
 [   1.4800319] fp ffffc00060ddfd20 vmem_alloc() at ffffc0000051127c netbsd:v=
 me
 m_alloc+0x84
 [   1.4900269] fp ffffc00060ddfd80 percpu_create() at ffffc000005019d4 netbs=
 d:
 percpu_create+0x3c
 [   1.5000283] fp ffffc00060ddfe00 pic_add() at ffffc00000003274 netbsd:pic_=
 ad
 d+0xf4
 [   1.5100278] fp ffffc00060ddfe40 bcm2836mp_intr_init() at ffffc0000001ad58=
  n
 etbsd:bcm2836mp_intr_init+0x90
 [   1.5200294] fp ffffc00060ddfe90 arm_fdt_cpu_hatch() at ffffc00000067e10 n=
 et
 bsd:arm_fdt_cpu_hatch+0x28
 [   1.5300288] fp ffffc00060ddfeb0 cpu_hatch() at ffffc000000971f4 netbsd:cp=
 u_
 hatch+0x8c
 [   1.5400298] fp 0000000000000000 cpu_mpstart() at ffffc00000001a88 netbsd:=
 cp
 u_mpstart+0x19c
 [   1.5400298] cpu2: End traceback...
 Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4:        ret
 db{2}>=20

 --=20
 Kouichi Hashikawa


 --Apple-Mail-3632CC7C-C285-4D44-AA8A-07E7A1A0178A
 Content-Type: text/html;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 <html><head><meta http-equiv=3D"content-type" content=3D"text/html; charset=3D=
 utf-8"></head><body dir=3D"auto"><div dir=3D"ltr">=EF=BB=BF<meta http-equiv=3D=
 "content-type" content=3D"text/html; charset=3Dutf-8"><div dir=3D"ltr">=EF=BB=
 =BF<meta http-equiv=3D"content-type" content=3D"text/html; charset=3Dutf-8">=
 <div dir=3D"ltr">&gt; State-Changed-Why:<br></div>&gt; This should be fixed i=
 n HEAD. Please update and report back.&nbsp;<div><div><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><b=
 r></span></div><div><span style=3D"-webkit-text-size-adjust: auto; caret-col=
 or: rgb(0, 0, 0); color: rgb(0, 0, 0);">I tried following image, but still p=
 anic.</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0,=
  0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto;=
  caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><a href=3D"http://nycdn.ne=
 tbsd.org/pub/NetBSD-daily/HEAD/202102202230Z/evbarm-aarch64/binary/gzimg/arm=
 64mbr.img.gz" dir=3D"ltr" x-apple-data-detectors=3D"true" x-apple-data-detec=
 tors-type=3D"link" x-apple-data-detectors-result=3D"0">http://nycdn.netbsd.o=
 rg/pub/NetBSD-daily/HEAD/202102202230Z/evbarm-aarch64/binary/gzimg/arm64mbr.=
 img.gz</a></span><br style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"></span><br style=3D"-w=
 ebkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0)=
 ;"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);"></span><br style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-=
 size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"></span><=
 br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color=
 : rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color:=
  rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.0000030] entropy: WARNI=
 NG: extracting entropy too early</span><br style=3D"-webkit-text-size-adjust=
 : auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 >[ &nbsp;&nbsp;1.4100223] panic: kernel diagnostic assertion "l-&gt;l_stat =3D=
 =3D LSONPROC" fail</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">ed: file "/ho=
 me/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227&nbsp;</span><br styl=
 e=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0=
 , 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0,=
  0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4200249] cpu2: Begin traceback=
 ...</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0=
 , 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4200249] tra=
 ce fp ffffc00060ddf9e0</span><br style=3D"-webkit-text-size-adjust: auto; ca=
 ret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-s=
 ize-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&=
 nbsp;1.4300234] fp ffffc00060ddfa10 vpanic() at ffffc0000050952c netbsd:vpan=
 ic+</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0=
 , 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">0x14c</span><br style=3D"-we=
 bkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);=
 "><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4300234] fp ffffc00060ddfa70 kern_asser=
 t() at ffffc0000075bbbc netbsd:ke</span><br style=3D"-webkit-text-size-adjus=
 t: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-we=
 bkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);=
 ">rn_assert+0x5c</span><br style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1=
 .4400250] fp ffffc00060ddfb00 sleepq_enqueue() at ffffc000004d4908 netbsd</s=
 pan><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);">:sleepq_enqueue+0x108</span><br sty=
 le=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(=
 0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0=
 , 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4500245] fp ffffc00060ddfb40 c=
 v_wait() at ffffc0000049ba88 netbsd:cv_wai</span><br style=3D"-webkit-text-s=
 ize-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span sty=
 le=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(=
 0, 0, 0);">t+0xe8</span><br style=3D"-webkit-text-size-adjust: auto; caret-c=
 olor: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;=
 1.4600255] fp ffffc00060ddfb80 xc_wait() at ffffc00000513498 netbsd:xc_wai</=
 span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);">t+0xb0</span><br style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><s=
 pan style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4700256] fp ffffc00060ddfbc0 percpu_backen=
 d_alloc() at ffffc00000501240&nbsp;</span><br style=3D"-webkit-text-size-adj=
 ust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-=
 webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">netbsd:percpu_backend_alloc+0x150</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.4800319] fp ffffc00060ddfc40 vmem_xalloc() at ffffc000=
 00510e44 netbsd:vm</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">em_xalloc+0x6=
 ac</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0,=
  0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; ca=
 ret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4800319] fp f=
 fffc00060ddfd20 vmem_alloc() at ffffc0000051127c netbsd:vme</span><br style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0=
 ); color: rgb(0, 0, 0);">m_alloc+0x84</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.4900269] fp ffffc00060ddfd80 percpu_create() at ffffc0=
 00005019d4 netbsd:</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">percpu_create=
 +0x3c</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0,=
  0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto;=
  caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5000283] f=
 p ffffc00060ddfe00 pic_add() at ffffc00000003274 netbsd:pic_ad</span><br sty=
 le=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(=
 0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0=
 , 0, 0); color: rgb(0, 0, 0);">d+0xf4</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.5100278] fp ffffc00060ddfe40 bcm2836mp_intr_init() at f=
 fffc0000001ad58 n</span><br style=3D"-webkit-text-size-adjust: auto; caret-c=
 olor: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">etbsd:bcm2836m=
 p_intr_init+0x90</span><br style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1=
 .5200294] fp ffffc00060ddfe90 arm_fdt_cpu_hatch() at ffffc00000067e10 net</s=
 pan><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);">bsd:arm_fdt_cpu_hatch+0x28</span><b=
 r style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color:=
  rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5300288] fp ffffc00060ddf=
 eb0 cpu_hatch() at ffffc000000971f4 netbsd:cpu_</span><br style=3D"-webkit-t=
 ext-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><spa=
 n style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color:=
  rgb(0, 0, 0);">hatch+0x8c</span><br style=3D"-webkit-text-size-adjust: auto=
 ; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-te=
 xt-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nb=
 sp;&nbsp;1.5400298] fp 0000000000000000 cpu_mpstart() at ffffc00000001a88 ne=
 tbsd:cp</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: aut=
 o; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">u_mpstart+0x19c</span><b=
 r style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color:=
  rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5400298] cpu2: End traceb=
 ack...</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0=
 , 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto=
 ; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">Stopped in pid 0.26 (syst=
 em) at netbsd:cpu_Debugger+0x4: &nbsp;&nbsp;&nbsp;&nbsp;&nbsp;&nbsp;&nbsp;re=
 t</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0=
 ); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; care=
 t-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">db{2}&gt;&nbsp;</span><br><br><=
 div dir=3D"ltr"><span style=3D"background-color: rgba(255, 255, 255, 0);">--=
 &nbsp;</span><div><span style=3D"background-color: rgba(255, 255, 255, 0);">=
 Kouichi Hashikawa</span></div><div><span style=3D"background-color: rgba(255=
 , 255, 255, 0);"><br></span></div></div></div></div></div></div></body></htm=
 l>=

 --Apple-Mail-3632CC7C-C285-4D44-AA8A-07E7A1A0178A--

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: kern-bug-people@netbsd.org, netbsd-bugs@netbsd.org,
 gnats-admin@netbsd.org, skrll@netbsd.org
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Sun, 21 Feb 2021 20:33:40 +0900

 --Apple-Mail-5304757D-4826-4C32-9580-BA0789CC78EA
 Content-Type: text/plain;
 	charset=us-ascii
 Content-Transfer-Encoding: quoted-printable

 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.=20

 I tried following image, but still panic.
 http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/202102202230Z/evbarm-aarch64/b=
 inary/gzimg/arm64mbr.img.gz



 [   1.0000030] entropy: WARNING: extracting entropy too early
 [   1.4100223] panic: kernel diagnostic assertion "l->l_stat =3D=3D LSONPROC=
 " fail
 ed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227=20
 [   1.4200249] cpu2: Begin traceback...
 [   1.4200249] trace fp ffffc00060ddf9e0
 [   1.4300234] fp ffffc00060ddfa10 vpanic() at ffffc0000050952c netbsd:vpani=
 c+
 0x14c
 [   1.4300234] fp ffffc00060ddfa70 kern_assert() at ffffc0000075bbbc netbsd:=
 ke
 rn_assert+0x5c
 [   1.4400250] fp ffffc00060ddfb00 sleepq_enqueue() at ffffc000004d4908 netb=
 sd
 :sleepq_enqueue+0x108
 [   1.4500245] fp ffffc00060ddfb40 cv_wait() at ffffc0000049ba88 netbsd:cv_w=
 ai
 t+0xe8
 [   1.4600255] fp ffffc00060ddfb80 xc_wait() at ffffc00000513498 netbsd:xc_w=
 ai
 t+0xb0
 [   1.4700256] fp ffffc00060ddfbc0 percpu_backend_alloc() at ffffc0000050124=
 0=20
 netbsd:percpu_backend_alloc+0x150
 [   1.4800319] fp ffffc00060ddfc40 vmem_xalloc() at ffffc00000510e44 netbsd:=
 vm
 em_xalloc+0x6ac
 [   1.4800319] fp ffffc00060ddfd20 vmem_alloc() at ffffc0000051127c netbsd:v=
 me
 m_alloc+0x84
 [   1.4900269] fp ffffc00060ddfd80 percpu_create() at ffffc000005019d4 netbs=
 d:
 percpu_create+0x3c
 [   1.5000283] fp ffffc00060ddfe00 pic_add() at ffffc00000003274 netbsd:pic_=
 ad
 d+0xf4
 [   1.5100278] fp ffffc00060ddfe40 bcm2836mp_intr_init() at ffffc0000001ad58=
  n
 etbsd:bcm2836mp_intr_init+0x90
 [   1.5200294] fp ffffc00060ddfe90 arm_fdt_cpu_hatch() at ffffc00000067e10 n=
 et
 bsd:arm_fdt_cpu_hatch+0x28
 [   1.5300288] fp ffffc00060ddfeb0 cpu_hatch() at ffffc000000971f4 netbsd:cp=
 u_
 hatch+0x8c
 [   1.5400298] fp 0000000000000000 cpu_mpstart() at ffffc00000001a88 netbsd:=
 cp
 u_mpstart+0x19c
 [   1.5400298] cpu2: End traceback...
 Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4:        ret
 db{2}>=20

 --=20
 Kouichi Hashikawa


 --Apple-Mail-5304757D-4826-4C32-9580-BA0789CC78EA
 Content-Type: text/html;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 <html><head><meta http-equiv=3D"content-type" content=3D"text/html; charset=3D=
 utf-8"></head><body dir=3D"auto"><div dir=3D"ltr">&gt; State-Changed-Why:<br=
 ></div>&gt; This should be fixed in HEAD. Please update and report back.&nbs=
 p;<div><div><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);"><br></span></div><div><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">I t=
 ried following image, but still panic.</span><br style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);"><a href=3D"http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/202102202230Z=
 /evbarm-aarch64/binary/gzimg/arm64mbr.img.gz" dir=3D"ltr" x-apple-data-detec=
 tors=3D"true" x-apple-data-detectors-type=3D"link" x-apple-data-detectors-re=
 sult=3D"0">http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/202102202230Z/evbar=
 m-aarch64/binary/gzimg/arm64mbr.img.gz</a></span><br style=3D"-webkit-text-s=
 ize-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span sty=
 le=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(=
 0, 0, 0);"></span><br style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"></span><br style=3D"-w=
 ebkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0)=
 ;"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);"></span><br style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-=
 size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;=
 &nbsp;1.0000030] entropy: WARNING: extracting entropy too early</span><br st=
 yle=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb=
 (0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4100223] panic: kernel diagn=
 ostic assertion "l-&gt;l_stat =3D=3D LSONPROC" fail</span><br style=3D"-webk=
 it-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">=
 <span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); co=
 lor: rgb(0, 0, 0);">ed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.=
 c", line 227&nbsp;</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp=
 ;1.4200249] cpu2: Begin traceback...</span><br style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"=
 -webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">[ &nbsp;&nbsp;1.4200249] trace fp ffffc00060ddf9e0</span><br style=3D"-w=
 ebkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0)=
 ;"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4300234] fp ffffc00060ddfa10 vpanic()=
  at ffffc0000050952c netbsd:vpanic+</span><br style=3D"-webkit-text-size-adj=
 ust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-=
 webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">0x14c</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rg=
 b(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.430023=
 4] fp ffffc00060ddfa70 kern_assert() at ffffc0000075bbbc netbsd:ke</span><br=
  style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: r=
 gb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rg=
 b(0, 0, 0); color: rgb(0, 0, 0);">rn_assert+0x5c</span><br style=3D"-webkit-=
 text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><sp=
 an style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color=
 : rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4400250] fp ffffc00060ddfb00 sleepq_enqueue=
 () at ffffc000004d4908 netbsd</span><br style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">:s=
 leepq_enqueue+0x108</span><br style=3D"-webkit-text-size-adjust: auto; caret=
 -color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size=
 -adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbs=
 p;1.4500245] fp ffffc00060ddfb40 cv_wait() at ffffc0000049ba88 netbsd:cv_wai=
 </span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0=
 ); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; care=
 t-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">t+0xe8</span><br style=3D"-webk=
 it-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">=
 <span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); co=
 lor: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4600255] fp ffffc00060ddfb80 xc_wait() a=
 t ffffc00000513498 netbsd:xc_wai</span><br style=3D"-webkit-text-size-adjust=
 : auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 >t+0xb0</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: aut=
 o; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4700256]=
  fp ffffc00060ddfbc0 percpu_backend_alloc() at ffffc00000501240&nbsp;</span>=
 <br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color=
 : rgb(0, 0, 0); color: rgb(0, 0, 0);">netbsd:percpu_backend_alloc+0x150</spa=
 n><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); co=
 lor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-col=
 or: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4800319] fp ffffc000=
 60ddfc40 vmem_xalloc() at ffffc00000510e44 netbsd:vm</span><br style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 ><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);">em_xalloc+0x6ac</span><br style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"=
 -webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">[ &nbsp;&nbsp;1.4800319] fp ffffc00060ddfd20 vmem_alloc() at ffffc000005=
 1127c netbsd:vme</span><br style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">m_alloc+0x84</s=
 pan><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4900269] fp ffffc00=
 060ddfd80 percpu_create() at ffffc000005019d4 netbsd:</span><br style=3D"-we=
 bkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);=
 "><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);">percpu_create+0x3c</span><br style=3D"-webkit-text-size=
 -adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.5000283] fp ffffc00060ddfe00 pic_add() at ffffc0000000=
 3274 netbsd:pic_ad</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">d+0xf4</span>=
 <br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color=
 : rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5100278] fp ffffc00060=
 ddfe40 bcm2836mp_intr_init() at ffffc0000001ad58 n</span><br style=3D"-webki=
 t-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><=
 span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); col=
 or: rgb(0, 0, 0);">etbsd:bcm2836mp_intr_init+0x90</span><br style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><s=
 pan style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5200294] fp ffffc00060ddfe90 arm_fdt_cpu_h=
 atch() at ffffc00000067e10 net</span><br style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">bs=
 d:arm_fdt_cpu_hatch+0x28</span><br style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-=
 size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;=
 &nbsp;1.5300288] fp ffffc00060ddfeb0 cpu_hatch() at ffffc000000971f4 netbsd:=
 cpu_</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0=
 , 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; c=
 aret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">hatch+0x8c</span><br style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0=
 ); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5400298] fp 0000000000000000 cpu_mp=
 start() at ffffc00000001a88 netbsd:cp</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">u_mpstart+0x19c</span><br style=3D"-webkit-text-size-adjust: auto; car=
 et-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-si=
 ze-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&n=
 bsp;1.5400298] cpu2: End traceback...</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4: &nbsp;&nbsp;&=
 nbsp;&nbsp;&nbsp;&nbsp;&nbsp;ret</span><br style=3D"-webkit-text-size-adjust=
 : auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 >db{2}&gt;&nbsp;</span><br><br><div dir=3D"ltr"><span style=3D"background-co=
 lor: rgba(255, 255, 255, 0);">--&nbsp;</span><div><span style=3D"background-=
 color: rgba(255, 255, 255, 0);">Kouichi Hashikawa</span></div><div><span sty=
 le=3D"background-color: rgba(255, 255, 255, 0);"><br></span></div></div></di=
 v></div></body></html>=

 --Apple-Mail-5304757D-4826-4C32-9580-BA0789CC78EA--

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: kern-bug-people@netbsd.org, netbsd-bugs@netbsd.org, skrll@netbsd.org
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Sun, 21 Feb 2021 21:38:41 +0900

 --Apple-Mail-A3575253-72CD-495A-B1E0-4DAF49D9B042
 Content-Type: text/plain;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 =EF=BB=BF
 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.=20

 I tried following image, but still panic.
 http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/202102202230Z/evbarm-aarch64/b=
 inary/gzimg/arm64mbr.img.gz



 [   1.0000030] entropy: WARNING: extracting entropy too early
 [   1.4100223] panic: kernel diagnostic assertion "l->l_stat =3D=3D LSONPROC=
 " fail
 ed: file "/home/source/ab/HEAD/src/sys/kern/kern_sleepq.c", line 227=20
 [   1.4200249] cpu2: Begin traceback...
 [   1.4200249] trace fp ffffc00060ddf9e0
 [   1.4300234] fp ffffc00060ddfa10 vpanic() at ffffc0000050952c netbsd:vpani=
 c+
 0x14c
 [   1.4300234] fp ffffc00060ddfa70 kern_assert() at ffffc0000075bbbc netbsd:=
 ke
 rn_assert+0x5c
 [   1.4400250] fp ffffc00060ddfb00 sleepq_enqueue() at ffffc000004d4908 netb=
 sd
 :sleepq_enqueue+0x108
 [   1.4500245] fp ffffc00060ddfb40 cv_wait() at ffffc0000049ba88 netbsd:cv_w=
 ai
 t+0xe8
 [   1.4600255] fp ffffc00060ddfb80 xc_wait() at ffffc00000513498 netbsd:xc_w=
 ai
 t+0xb0
 [   1.4700256] fp ffffc00060ddfbc0 percpu_backend_alloc() at ffffc0000050124=
 0=20
 netbsd:percpu_backend_alloc+0x150
 [   1.4800319] fp ffffc00060ddfc40 vmem_xalloc() at ffffc00000510e44 netbsd:=
 vm
 em_xalloc+0x6ac
 [   1.4800319] fp ffffc00060ddfd20 vmem_alloc() at ffffc0000051127c netbsd:v=
 me
 m_alloc+0x84
 [   1.4900269] fp ffffc00060ddfd80 percpu_create() at ffffc000005019d4 netbs=
 d:
 percpu_create+0x3c
 [   1.5000283] fp ffffc00060ddfe00 pic_add() at ffffc00000003274 netbsd:pic_=
 ad
 d+0xf4
 [   1.5100278] fp ffffc00060ddfe40 bcm2836mp_intr_init() at ffffc0000001ad58=
  n
 etbsd:bcm2836mp_intr_init+0x90
 [   1.5200294] fp ffffc00060ddfe90 arm_fdt_cpu_hatch() at ffffc00000067e10 n=
 et
 bsd:arm_fdt_cpu_hatch+0x28
 [   1.5300288] fp ffffc00060ddfeb0 cpu_hatch() at ffffc000000971f4 netbsd:cp=
 u_
 hatch+0x8c
 [   1.5400298] fp 0000000000000000 cpu_mpstart() at ffffc00000001a88 netbsd:=
 cp
 u_mpstart+0x19c
 [   1.5400298] cpu2: End traceback...
 Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4:        ret
 db{2}>=20

 --=20
 Kouichi Hashikawa


 --Apple-Mail-A3575253-72CD-495A-B1E0-4DAF49D9B042
 Content-Type: text/html;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 <html><head><meta http-equiv=3D"content-type" content=3D"text/html; charset=3D=
 utf-8"></head><body dir=3D"auto"><div dir=3D"ltr">=EF=BB=BF<meta http-equiv=3D=
 "content-type" content=3D"text/html; charset=3Dutf-8"><div dir=3D"ltr">&gt; S=
 tate-Changed-Why:<br></div>&gt; This should be fixed in HEAD. Please update a=
 nd report back.&nbsp;<div><div><span style=3D"-webkit-text-size-adjust: auto=
 ; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><br></span></div><div><sp=
 an style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color=
 : rgb(0, 0, 0);">I tried following image, but still panic.</span><br style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0=
 ); color: rgb(0, 0, 0);"><a href=3D"http://nycdn.netbsd.org/pub/NetBSD-daily=
 /HEAD/202102202230Z/evbarm-aarch64/binary/gzimg/arm64mbr.img.gz" dir=3D"ltr"=
  x-apple-data-detectors=3D"true" x-apple-data-detectors-type=3D"link" x-appl=
 e-data-detectors-result=3D"0">http://nycdn.netbsd.org/pub/NetBSD-daily/HEAD/=
 202102202230Z/evbarm-aarch64/binary/gzimg/arm64mbr.img.gz</a></span><br styl=
 e=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0=
 , 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0,=
  0, 0); color: rgb(0, 0, 0);"></span><br style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"></=
 span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"></span><br style=3D"-webkit-text-=
 size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span st=
 yle=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb=
 (0, 0, 0);">[ &nbsp;&nbsp;1.0000030] entropy: WARNING: extracting entropy to=
 o early</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: aut=
 o; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4100223]=
  panic: kernel diagnostic assertion "l-&gt;l_stat =3D=3D LSONPROC" fail</spa=
 n><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); co=
 lor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-col=
 or: rgb(0, 0, 0); color: rgb(0, 0, 0);">ed: file "/home/source/ab/HEAD/src/s=
 ys/kern/kern_sleepq.c", line 227&nbsp;</span><br style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.4200249] cpu2: Begin traceback...</span><br style=3D"-=
 webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0)=
 ; color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4200249] trace fp ffffc00060ddf9e0</=
 span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0);=
  color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4300234] fp ffffc=
 00060ddfa10 vpanic() at ffffc0000050952c netbsd:vpanic+</span><br style=3D"-=
 webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0)=
 ; color: rgb(0, 0, 0);">0x14c</span><br style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &=
 nbsp;&nbsp;1.4300234] fp ffffc00060ddfa70 kern_assert() at ffffc0000075bbbc n=
 etbsd:ke</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb=
 (0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: au=
 to; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">rn_assert+0x5c</span><b=
 r style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color:=
  rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4400250] fp ffffc00060ddf=
 b00 sleepq_enqueue() at ffffc000004d4908 netbsd</span><br style=3D"-webkit-t=
 ext-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><spa=
 n style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color:=
  rgb(0, 0, 0);">:sleepq_enqueue+0x108</span><br style=3D"-webkit-text-size-a=
 djust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.4500245] fp ffffc00060ddfb40 cv_wait() at ffffc0000049=
 ba88 netbsd:cv_wai</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">t+0xe8</span>=
 <br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color=
 : rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4600255] fp ffffc00060=
 ddfb80 xc_wait() at ffffc00000513498 netbsd:xc_wai</span><br style=3D"-webki=
 t-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><=
 span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); col=
 or: rgb(0, 0, 0);">t+0xb0</span><br style=3D"-webkit-text-size-adjust: auto;=
  caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-tex=
 t-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbs=
 p;&nbsp;1.4700256] fp ffffc00060ddfbc0 percpu_backend_alloc() at ffffc000005=
 01240&nbsp;</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">netbsd:percpu_backend_=
 alloc+0x150</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.480031=
 9] fp ffffc00060ddfc40 vmem_xalloc() at ffffc00000510e44 netbsd:vm</span><br=
  style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: r=
 gb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rg=
 b(0, 0, 0); color: rgb(0, 0, 0);">em_xalloc+0x6ac</span><br style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><s=
 pan style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); colo=
 r: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.4800319] fp ffffc00060ddfd20 vmem_alloc() a=
 t ffffc0000051127c netbsd:vme</span><br style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit=
 -text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">m_=
 alloc+0x84</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: r=
 gb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: a=
 uto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.490026=
 9] fp ffffc00060ddfd80 percpu_create() at ffffc000005019d4 netbsd:</span><br=
  style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: r=
 gb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rg=
 b(0, 0, 0); color: rgb(0, 0, 0);">percpu_create+0x3c</span><br style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 ><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5000283] fp ffffc00060ddfe00 pic_add() a=
 t ffffc00000003274 netbsd:pic_ad</span><br style=3D"-webkit-text-size-adjust=
 : auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-web=
 kit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"=
 >d+0xf4</span><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: aut=
 o; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5100278]=
  fp ffffc00060ddfe40 bcm2836mp_intr_init() at ffffc0000001ad58 n</span><br s=
 tyle=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rg=
 b(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb=
 (0, 0, 0); color: rgb(0, 0, 0);">etbsd:bcm2836mp_intr_init+0x90</span><br st=
 yle=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb=
 (0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(=
 0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5200294] fp ffffc00060ddfe90=
  arm_fdt_cpu_hatch() at ffffc00000067e10 net</span><br style=3D"-webkit-text=
 -size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span s=
 tyle=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rg=
 b(0, 0, 0);">bsd:arm_fdt_cpu_hatch+0x28</span><br style=3D"-webkit-text-size=
 -adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D=
 "-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0,=
  0);">[ &nbsp;&nbsp;1.5300288] fp ffffc00060ddfeb0 cpu_hatch() at ffffc00000=
 0971f4 netbsd:cpu_</span><br style=3D"-webkit-text-size-adjust: auto; caret-=
 color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-=
 adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">hatch+0x8c</s=
 pan><br style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);"><span style=3D"-webkit-text-size-adjust: auto; caret-co=
 lor: rgb(0, 0, 0); color: rgb(0, 0, 0);">[ &nbsp;&nbsp;1.5400298] fp 0000000=
 000000000 cpu_mpstart() at ffffc00000001a88 netbsd:cp</span><br style=3D"-we=
 bkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);=
 "><span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); c=
 olor: rgb(0, 0, 0);">u_mpstart+0x19c</span><br style=3D"-webkit-text-size-ad=
 just: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span style=3D"=
 -webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">[ &nbsp;&nbsp;1.5400298] cpu2: End traceback...</span><br style=3D"-webk=
 it-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">=
 <span style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); co=
 lor: rgb(0, 0, 0);">Stopped in pid 0.26 (system) at netbsd:cpu_Debugger+0x4:=
  &nbsp;&nbsp;&nbsp;&nbsp;&nbsp;&nbsp;&nbsp;ret</span><br style=3D"-webkit-te=
 xt-size-adjust: auto; caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><span=
  style=3D"-webkit-text-size-adjust: auto; caret-color: rgb(0, 0, 0); color: r=
 gb(0, 0, 0);">db{2}&gt;&nbsp;</span><br><br><div dir=3D"ltr"><span style=3D"=
 background-color: rgba(255, 255, 255, 0);">--&nbsp;</span><div><span style=3D=
 "background-color: rgba(255, 255, 255, 0);">Kouichi Hashikawa</span></div><d=
 iv><span style=3D"background-color: rgba(255, 255, 255, 0);"><br></span></di=
 v></div></div></div></div></body></html>=

 --Apple-Mail-A3575253-72CD-495A-B1E0-4DAF49D9B042--

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: skrll@netbsd.org, mlelstv@serpens.de
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Tue, 2 Mar 2021 01:18:27 +0900

 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.

 I build old code,
 until -D2020.07.28.20.12.00: panic don=E2=80=99t occurred.
 from -D2020.07.28.20.20.00: panic occurred.

 When -D2020.07.28.20.20.00 code + src/sys/crypto/cprng_fast/cprng_fast.c 1.1=
 6 -> 1.15: panic don=E2=80=99t occurred.

 When latest cvs code + src/sys/crypto/cprng_fast/cprng_fast.c 1.16 -> 1.15: p=
 anic don=E2=80=99t occurred.



 --=20
 Kouichi Hashikawa

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: skrll@netbsd.org, mlelstv@serpens.de, gnats-admin@netbsd.org
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Tue, 2 Mar 2021 20:18:11 +0900

 =EF=BB=BF
 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.

 I build old code,
 until -D2020.07.28.20.12.00: panic don=E2=80=99t occurred.
 from -D2020.07.28.20.20.00: panic occurred.

 When -D2020.07.28.20.20.00 code + src/sys/crypto/cprng_fast/cprng_fast.c 1.1=
 6 -> 1.15: panic don=E2=80=99t occurred.

 When latest cvs code + src/sys/crypto/cprng_fast/cprng_fast.c 1.16 -> 1.15: p=
 anic don=E2=80=99t occurred.



 --=20
 Kouichi Hashikawa

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: skrll@netbsd.org, mlelstv@serpens.de, gnats-admin@netbsd.org,
 kern-bug-people@netbsd.org
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Wed, 3 Mar 2021 02:46:53 +0900

 > State-Changed-Why:
 > This should be fixed in HEAD. Please update and report back.

 I build old code,
 until -D2020.07.28.20.12.00: panic don=E2=80=99t occurred.
 from -D2020.07.28.20.20.00: panic occurred.

 https://releng.netbsd.org/b5reports/evbarm-aarch64/commits-2020.07.html
 --------
 commit 2020.07.28.20.05.33 riastradh src/sys/crypto/chacha/arch/arm/chacha_n=
 eon.c 1.6
 commit 2020.07.28.20.08.48 riastradh src/sys/crypto/chacha/arch/arm/chacha_n=
 eon.c 1.7
 commit 2020.07.28.20.08.48 riastradh src/sys/crypto/chacha/arch/arm/chacha_n=
 eon.h 1.3
 commit 2020.07.28.20.08.48 riastradh src/sys/crypto/chacha/arch/arm/chacha_n=
 eon_32.S 1.1
 commit 2020.07.28.20.08.48 riastradh src/sys/crypto/chacha/arch/arm/files.ch=
 acha_arm 1.3
 commit 2020.07.28.20.08.48 riastradh src/tests/sys/crypto/chacha/Makefile 1.=
 3
 commit 2020.07.28.20.11.09 riastradh src/sys/crypto/aes/arch/arm/aes_neon.c 1=
 .4
 commit 2020.07.28.20.11.09 riastradh src/sys/crypto/aes/arch/arm/aes_neon_im=
 pl.h 1.2
 commit 2020.07.28.20.11.09 riastradh src/sys/crypto/aes/arch/arm/aes_neon_su=
 br.c 1.4
 commit 2020.07.28.20.11.09 riastradh src/sys/crypto/aes/arch/arm/arm_neon.h 1=
 .7
 commit 2020.07.28.20.15.07 riastradh src/sys/crypto/cprng_fast/cprng_fast.c 1=
 .16
 commit 2020.07.28.20.15.07 riastradh src/sys/crypto/cprng_fast/files.cprng_f=
 ast 1.3
 commit 2020.07.28.20.15.07 riastradh src/sys/kern/files.kern 1.50
 commit 2020.07.28.20.15.07 riastradh src/sys/rump/kern/lib/libcrypto/Makefil=
 e 1.13
 commit 2020.07.28.20.15.07 riastradh src/sys/rump/librump/rumpkern/Makefile.=
 rumpkern 1.184
 --------


 When -D2020.07.28.20.20.00 code + src/sys/crypto/cprng_fast/cprng_fast.c 1.1=
 6 -> 1.15: panic don=E2=80=99t occurred.

 When latest cvs code + src/sys/crypto/cprng_fast/cprng_fast.c 1.16 -> 1.15: p=
 anic don=E2=80=99t occurred.



 --=20
 Kouichi Hashikawa=

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: kern-bug-people@netbsd.org, gnats-admin@netbsd.org, skrll@netbsd.org,
 mlelstv@serpens.de
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Fri, 12 Mar 2021 02:50:28 +0900

 I found following comment in src/sys/net/route.c,
 * We can't have struct route as percpu data because it can be destroyed
 * over a memory enlargement processing of percpu.
 I change percpu_create(sizeof(struct cprng_fast) to percpu_create(sizeof(str=
 uc
 t cprng_fast *),
 kernel can boot.

 In src/sys/arch/arm/pic/pic.c, use percpu_create(sizeof(struct pic_percpu) a=
 lso.

 --- src/sys/crypto/cprng_fast/cprng_fast.c-1.16 2020-12-21 16:19:54.00000000=
 0=20
 +0900
 +++ src/sys/crypto/cprng_fast/cprng_fast.c      2021-03-11 16:44:11.89642563=
 8=20
 +0900
 @@ -70,11 +70,25 @@
 static percpu_t        *cprng_fast_percpu      __read_mostly;
 static void    *cprng_fast_softint     __read_mostly;

 +static inline struct cprng_fast *
 +cprng_percpu_getref(percpu_t *pc)
 +{
 +
 +       return *(struct cprng_fast **)percpu_getref(pc);
 +}
 +
 +static inline void
 +cprng_percpu_putref(percpu_t *pc)
 +{
 +
 +       percpu_putref(pc);
 +}
 +
 void
 cprng_fast_init(void)
 {

 -       cprng_fast_percpu =3D percpu_create(sizeof(struct cprng_fast),
 +       cprng_fast_percpu =3D percpu_create(sizeof(struct cprng_fast *),
           cprng_fast_init_cpu, NULL, NULL);
       cprng_fast_softint =3D softint_establish(SOFTINT_SERIAL|SOFTINT_MPSAFE=
 ,
           &cprng_fast_intr, NULL);
 @@ -83,9 +97,12 @@
 static void
 cprng_fast_init_cpu(void *p, void *arg __unused, struct cpu_info *ci)
 {
 -       struct cprng_fast *const cprng =3D p;
 +       struct cprng_fast **const cprngp =3D p;
       uint8_t seed[CPRNG_FAST_SEED_BYTES];

 +       *cprngp =3D kmem_zalloc(sizeof(**cprngp), KM_SLEEP);
 +       struct cprng_fast *const cprng =3D *cprngp;
 +
       cprng->epoch =3D entropy_epoch();
       cprng_strong(kern_cprng, seed, sizeof seed, 0);
       cprng_fast_seed(cprng, seed);
 @@ -103,7 +120,7 @@
       struct cprng_fast *cprng;
       int s;

 -       *cprngp =3D cprng =3D percpu_getref(cprng_fast_percpu);
 +       *cprngp =3D cprng =3D cprng_percpu_getref(cprng_fast_percpu);
       s =3D splvm();

       if (__predict_false(cprng->epoch !=3D entropy_epoch()))
 @@ -116,7 +133,7 @@
 cprng_fast_put(struct cprng_fast *cprng, int s)
 {

 -       KASSERT((cprng =3D=3D percpu_getref(cprng_fast_percpu)) &&
 +       KASSERT((cprng =3D=3D cprng_percpu_getref(cprng_fast_percpu)) &&
           (percpu_putref(cprng_fast_percpu), true));
       splx(s);
       percpu_putref(cprng_fast_percpu);
 @@ -139,7 +156,7 @@

       cprng_strong(kern_cprng, seed, sizeof(seed), 0);

 -       cprng =3D percpu_getref(cprng_fast_percpu);
 +       cprng =3D cprng_percpu_getref(cprng_fast_percpu);
       s =3D splvm();
       cprng_fast_seed(cprng, seed);
       cprng->epoch =3D epoch;


 (missing correction?)
 --- src/sys/net/if_l2tp.c-dist  2020-12-21 16:20:48.000000000 +0900
 +++ src/sys/net/if_l2tp.c       2021-03-12 02:34:27.644208958 +0900
 @@ -411,7 +411,7 @@
       }

       IF_ENQUEUE(ifq, m);
 -       percpu_putref(sc->l2tp_ifq_percpu);
 +       l2tp_ifq_percpu_putref(sc->l2tp_ifq_percpu);
       softint_schedule(sc->l2tp_si);
       /* counter is incremented in l2tpintr() */
       splx(s);


 --=20
 Kouichi Hashikawa


From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: kern-bug-people@netbsd.org, gnats-admin@netbsd.org, mlelstv@serpens.de
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Sat, 3 Apr 2021 02:53:23 +0900

 --Apple-Mail-FC2AB20F-18B9-4B76-971B-62C05C83121C
 Content-Type: text/plain;
 	charset=us-ascii
 Content-Transfer-Encoding: 7bit

 Kernel from  -D2021.03.27.12.00.00 source, panic still occurred.

 Kernel from  -D2021.03.27.12.00.00 source, 
 panic do not occurred.

 I think this problem is fixed.


 -- 
 Kouichi Hashikawa
 --Apple-Mail-FC2AB20F-18B9-4B76-971B-62C05C83121C
 Content-Type: text/html;
 	charset=utf-8
 Content-Transfer-Encoding: 7bit

 <html><head><meta http-equiv="content-type" content="text/html; charset=utf-8"></head><body dir="auto">Kernel from &nbsp;-D2021.03.27.12.00.00 source, panic still occurred.<div><span style="caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);"><br></span></div><div><span style="caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">Kernel from &nbsp;-D2021.03.27.12.00.00 source,&nbsp;</span></div><div><font color="#000000"><span style="caret-color: rgb(0, 0, 0);">panic do not occurred.</span></font></div><div><font color="#000000"><span style="caret-color: rgb(0, 0, 0);"><br></span></font></div><div><font color="#000000"><span style="caret-color: rgb(0, 0, 0);">I think this problem is fixed.</span></font></div><div><div><div><div><br><br><div dir="ltr"><span style="background-color: rgba(255, 255, 255, 0);">--&nbsp;</span><div><span style="background-color: rgba(255, 255, 255, 0);">Kouichi Hashikawa</span></div></div></div></div></div></div></body></html>
 --Apple-Mail-FC2AB20F-18B9-4B76-971B-62C05C83121C--

From: Kouichi Hashikawa <hashikaw@mail.ru>
To: gnats-bugs@netbsd.org
Cc: kern-bug-people@netbsd.org, gnats-admin@netbsd.org, mlelstv@serpens.de
Subject: Re: kern/55889 (panic when boot GENERIC64 kernel on RaspberryPi4 (without  RPi4_UEFI_Firmware))
Date: Sat, 3 Apr 2021 02:54:20 +0900

 --Apple-Mail-30330A89-2E94-483B-AE99-91D7B6556CC1
 Content-Type: text/plain;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 =EF=BB=BFKernel from  -D2021.03.27.12.00.00 source, panic still occurred.

 Kernel from  -D2021.03.27.12.20.00 source,=20
 panic do not occurred.

 I think this problem is fixed.


 --=20
 Kouichi Hashikawa=

 --Apple-Mail-30330A89-2E94-483B-AE99-91D7B6556CC1
 Content-Type: text/html;
 	charset=utf-8
 Content-Transfer-Encoding: quoted-printable

 <html><head><meta http-equiv=3D"content-type" content=3D"text/html; charset=3D=
 utf-8"></head><body dir=3D"auto"><div dir=3D"ltr">=EF=BB=BF<meta http-equiv=3D=
 "content-type" content=3D"text/html; charset=3Dutf-8">Kernel from &nbsp;-D20=
 21.03.27.12.00.00 source, panic still occurred.<div><span style=3D"caret-col=
 or: rgb(0, 0, 0); color: rgb(0, 0, 0);"><br></span></div><div><span style=3D=
 "caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0);">Kernel from &nbsp;-D2021.0=
 3.27.12.2</span><span style=3D"caret-color: rgb(0, 0, 0); color: rgb(0, 0, 0=
 );">0.00 source,&nbsp;</span></div><div><font color=3D"#000000"><span style=3D=
 "caret-color: rgb(0, 0, 0);">panic do not occurred.</span></font></div><div>=
 <font color=3D"#000000"><span style=3D"caret-color: rgb(0, 0, 0);"><br></spa=
 n></font></div><div><font color=3D"#000000"><span style=3D"caret-color: rgb(=
 0, 0, 0);">I think this problem is fixed.</span></font></div><div><div><div>=
 <div><br><br><div dir=3D"ltr"><span style=3D"background-color: rgba(255, 255=
 , 255, 0);">--&nbsp;</span><div><span style=3D"background-color: rgba(255, 2=
 55, 255, 0);">Kouichi Hashikawa</span></div></div></div></div></div></div></=
 div></body></html>=

 --Apple-Mail-30330A89-2E94-483B-AE99-91D7B6556CC1--

State-Changed-From-To: feedback->closed
State-Changed-By: skrll@NetBSD.org
State-Changed-When: Sat, 03 Apr 2021 07:28:49 +0000
State-Changed-Why:
Fixed (for now)


>Unformatted:

NetBSD Home
NetBSD PR Database Search

(Contact us) $NetBSD: query-full-pr,v 1.46 2020/01/03 16:35:01 leot Exp $
$NetBSD: gnats_config.sh,v 1.9 2014/08/02 14:16:04 spz Exp $
Copyright © 1994-2020 The NetBSD Foundation, Inc. ALL RIGHTS RESERVED.