<p dir="auto">I cannot reproduce it myself, but from windows-386-gce builder <a href="http://build.golang.org/log/e3bf7d994667518abb7f2a2f0064257d8c373927" rel="nofollow">http://build.golang.org/log/e3bf7d994667518abb7f2a2f0064257d8c373927</a> while building <a class="commit-link" data-hovercard-type="commit" data-hovercard-url="https://github.com/golang/go/commit/56a7c5b95c01ccf23914ddb70193c3943ae5aaa0/hovercard" href="https://github.com/golang/go/commit/56a7c5b95c01ccf23914ddb70193c3943ae5aaa0"><tt>56a7c5b</tt></a></p>
<div class="snippet-clipboard-content notranslate position-relative overflow-auto" data-snippet-clipboard-copy-content="fatal error: unexpected signal during runtime execution
[signal 0xc0000005 code=0x0 addr=0x2140c00 pc=0x40d8c1]

runtime stack:
runtime.throw(0x5ff288, 0x2a)
    C:/workdir/go/src/runtime/panic.go:543 +0x7f
runtime.sigpanic()
    C:/workdir/go/src/runtime/signal_windows.go:157 +0x5c
runtime.gcmarkwb_m(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:73 +0xb1
runtime.writebarrierptr_nostore1.func1()
    C:/workdir/go/src/runtime/mbarrier.go:107 +0x117
runtime.systemstack(0x32a7fdfc)
    C:/workdir/go/src/runtime/asm_386.s:283 +0x81
runtime.writebarrierptr_nostore1(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:108 +0x56
runtime.writebarrierptr(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:131 +0x7f
runtime.writebarrierslice(0x3280000c, 0x32800218, 0x6933, 0xfde8)
    C:/workdir/go/src/runtime/mbarrier.go:207 +0x1e
runtime.traceEvent(0x15, 0x0, 0x32a7fee4, 0x1, 0x1)
    C:/workdir/go/src/runtime/trace.go:502 +0x5b2
runtime.traceGoUnpark(0x12215080, 0x0)
    C:/workdir/go/src/runtime/trace.go:793 +0x75
runtime.findrunnable(0x12212a00)
    C:/workdir/go/src/runtime/proc1.go:1345 +0x251
runtime.schedule()
    C:/workdir/go/src/runtime/proc1.go:1515 +0x1dd
runtime.park_m(0x12215080)
    C:/workdir/go/src/runtime/proc1.go:1574 +0x161
runtime.mcall(0x0)
    C:/workdir/go/src/runtime/asm_386.s:210 +0x47

goroutine 1 [chan receive]:
testing.RunTests(0x620844, 0x6b83e0, 0xe, 0xe, 0x12246001)
    C:/workdir/go/src/testing/testing.go:561 +0x884
testing.(*M).Run(0x12206360, 0x6cf540)
    C:/workdir/go/src/testing/testing.go:490 +0x6b
main.main()
    runtime/pprof/_test/_testmain.go:82 +0x177

goroutine 58 [runnable]:
runtime/pprof_test.TestTraceStress(0x18a9dd40)
    C:/workdir/go/src/runtime/pprof/trace_test.go:149 +0x3af
testing.tRunner(0x18a9dd40, 0x6b8464)
    C:/workdir/go/src/testing/testing.go:452 +0xa6
created by testing.RunTests
    C:/workdir/go/src/testing/testing.go:560 +0x852

goroutine 41 [select (no cases)]:
runtime/pprof_test.TestTraceSymbolize.func1()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:38 +0x1e
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:39 +0x178

goroutine 60 [syscall, locked to thread]:
syscall.Syscall6(0x77433e93, 0x5, 0x194, 0x1268cfcf, 0x1, 0x1268cf38, 0x0, 0x0, 0x40bbd6, 0x6be720, ...)
    C:/workdir/go/src/runtime/syscall_windows.go:139 +0x4b
syscall.ReadFile(0x194, 0x1268cfcf, 0x1, 0x1, 0x1268cf38, 0x0, 0x0, 0x0)
    C:/workdir/go/src/syscall/zsyscall_windows.go:283 +0xa0
syscall.Read(0x194, 0x1268cfcf, 0x1, 0x1, 0xf69, 0x0, 0x0)
    C:/workdir/go/src/syscall/syscall_windows.go:286 +0x64
os.(*File).read(0x1221e658, 0x1268cfcf, 0x1, 0x1, 0x0, 0x0, 0x0)
    C:/workdir/go/src/os/file_windows.go:300 +0x106
os.(*File).Read(0x1221e658, 0x1268cfcf, 0x1, 0x1, 0x0, 0x0, 0x0)
    C:/workdir/go/src/os/file.go:95 +0x72
runtime/pprof_test.TestTraceStress.func3(0x1221e658, 0x126a7940, 0x1228c9a0)
    C:/workdir/go/src/runtime/pprof/trace_test.go:120 +0x5b
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:123 +0x1ff

goroutine 42 [chan send (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func2()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:42 +0x3e
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:43 +0x18d

goroutine 43 [chan receive (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func3()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:46 +0x36
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:47 +0x1a2

goroutine 62 [runnable, locked to thread]:
runtime.Gosched()
    C:/workdir/go/src/runtime/proc.go:166 +0x10
runtime/pprof_test.TestTraceStress.func4(0x126a7940)
    C:/workdir/go/src/runtime/pprof/trace_test.go:141 +0xb4
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:144 +0x371

goroutine 59 [chan receive]:
runtime/pprof_test.TestTraceStress.func1(0x126a7940, 0x1228c9a0)
    C:/workdir/go/src/runtime/pprof/trace_test.go:104 +0x38
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:106 +0xa3

goroutine 61 [trace reader (blocked)]:
runtime.ReadTrace(0x0, 0x0, 0x0)
    C:/workdir/go/src/runtime/trace.go:313 +0x1d9
runtime/pprof.StartTrace.func1(0x3b0c58, 0x18a9dda0)
    C:/workdir/go/src/runtime/pprof/pprof.go:629 +0x21
created by runtime/pprof.StartTrace
    C:/workdir/go/src/runtime/pprof/pprof.go:635 +0x70
FAIL    runtime/pprof   8.670s"><pre class="notranslate"><code class="notranslate">fatal error: unexpected signal during runtime execution
[signal 0xc0000005 code=0x0 addr=0x2140c00 pc=0x40d8c1]

runtime stack:
runtime.throw(0x5ff288, 0x2a)
    C:/workdir/go/src/runtime/panic.go:543 +0x7f
runtime.sigpanic()
    C:/workdir/go/src/runtime/signal_windows.go:157 +0x5c
runtime.gcmarkwb_m(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:73 +0xb1
runtime.writebarrierptr_nostore1.func1()
    C:/workdir/go/src/runtime/mbarrier.go:107 +0x117
runtime.systemstack(0x32a7fdfc)
    C:/workdir/go/src/runtime/asm_386.s:283 +0x81
runtime.writebarrierptr_nostore1(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:108 +0x56
runtime.writebarrierptr(0x3280000c, 0x32800218)
    C:/workdir/go/src/runtime/mbarrier.go:131 +0x7f
runtime.writebarrierslice(0x3280000c, 0x32800218, 0x6933, 0xfde8)
    C:/workdir/go/src/runtime/mbarrier.go:207 +0x1e
runtime.traceEvent(0x15, 0x0, 0x32a7fee4, 0x1, 0x1)
    C:/workdir/go/src/runtime/trace.go:502 +0x5b2
runtime.traceGoUnpark(0x12215080, 0x0)
    C:/workdir/go/src/runtime/trace.go:793 +0x75
runtime.findrunnable(0x12212a00)
    C:/workdir/go/src/runtime/proc1.go:1345 +0x251
runtime.schedule()
    C:/workdir/go/src/runtime/proc1.go:1515 +0x1dd
runtime.park_m(0x12215080)
    C:/workdir/go/src/runtime/proc1.go:1574 +0x161
runtime.mcall(0x0)
    C:/workdir/go/src/runtime/asm_386.s:210 +0x47

goroutine 1 [chan receive]:
testing.RunTests(0x620844, 0x6b83e0, 0xe, 0xe, 0x12246001)
    C:/workdir/go/src/testing/testing.go:561 +0x884
testing.(*M).Run(0x12206360, 0x6cf540)
    C:/workdir/go/src/testing/testing.go:490 +0x6b
main.main()
    runtime/pprof/_test/_testmain.go:82 +0x177

goroutine 58 [runnable]:
runtime/pprof_test.TestTraceStress(0x18a9dd40)
    C:/workdir/go/src/runtime/pprof/trace_test.go:149 +0x3af
testing.tRunner(0x18a9dd40, 0x6b8464)
    C:/workdir/go/src/testing/testing.go:452 +0xa6
created by testing.RunTests
    C:/workdir/go/src/testing/testing.go:560 +0x852

goroutine 41 [select (no cases)]:
runtime/pprof_test.TestTraceSymbolize.func1()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:38 +0x1e
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:39 +0x178

goroutine 60 [syscall, locked to thread]:
syscall.Syscall6(0x77433e93, 0x5, 0x194, 0x1268cfcf, 0x1, 0x1268cf38, 0x0, 0x0, 0x40bbd6, 0x6be720, ...)
    C:/workdir/go/src/runtime/syscall_windows.go:139 +0x4b
syscall.ReadFile(0x194, 0x1268cfcf, 0x1, 0x1, 0x1268cf38, 0x0, 0x0, 0x0)
    C:/workdir/go/src/syscall/zsyscall_windows.go:283 +0xa0
syscall.Read(0x194, 0x1268cfcf, 0x1, 0x1, 0xf69, 0x0, 0x0)
    C:/workdir/go/src/syscall/syscall_windows.go:286 +0x64
os.(*File).read(0x1221e658, 0x1268cfcf, 0x1, 0x1, 0x0, 0x0, 0x0)
    C:/workdir/go/src/os/file_windows.go:300 +0x106
os.(*File).Read(0x1221e658, 0x1268cfcf, 0x1, 0x1, 0x0, 0x0, 0x0)
    C:/workdir/go/src/os/file.go:95 +0x72
runtime/pprof_test.TestTraceStress.func3(0x1221e658, 0x126a7940, 0x1228c9a0)
    C:/workdir/go/src/runtime/pprof/trace_test.go:120 +0x5b
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:123 +0x1ff

goroutine 42 [chan send (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func2()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:42 +0x3e
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:43 +0x18d

goroutine 43 [chan receive (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func3()
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:46 +0x36
created by runtime/pprof_test.TestTraceSymbolize
    C:/workdir/go/src/runtime/pprof/trace_stack_test.go:47 +0x1a2

goroutine 62 [runnable, locked to thread]:
runtime.Gosched()
    C:/workdir/go/src/runtime/proc.go:166 +0x10
runtime/pprof_test.TestTraceStress.func4(0x126a7940)
    C:/workdir/go/src/runtime/pprof/trace_test.go:141 +0xb4
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:144 +0x371

goroutine 59 [chan receive]:
runtime/pprof_test.TestTraceStress.func1(0x126a7940, 0x1228c9a0)
    C:/workdir/go/src/runtime/pprof/trace_test.go:104 +0x38
created by runtime/pprof_test.TestTraceStress
    C:/workdir/go/src/runtime/pprof/trace_test.go:106 +0xa3

goroutine 61 [trace reader (blocked)]:
runtime.ReadTrace(0x0, 0x0, 0x0)
    C:/workdir/go/src/runtime/trace.go:313 +0x1d9
runtime/pprof.StartTrace.func1(0x3b0c58, 0x18a9dda0)
    C:/workdir/go/src/runtime/pprof/pprof.go:629 +0x21
created by runtime/pprof.StartTrace
    C:/workdir/go/src/runtime/pprof/pprof.go:635 +0x70
FAIL    runtime/pprof   8.670s
</code></pre></div>
<p dir="auto">I also have couple of questions about the stack trace:</p>
<ul dir="auto">
<li>It looks like our exception handler got fired because of EXCEPTION_ACCESS_VIOLATION (see signal 0xc0000005). The source code line where it happened must be mbarrier.go:73 - it is right before signal_windows.go:157 (runtime.sigpanic). Looking at that line: "if ptr != 0 &amp;&amp; inheap(ptr) {", I don't see how it is possible for EXCEPTION_ACCESS_VIOLATION to be raised here. Can someone explain?</li>
<li>Also "runtime stack:" starts with runtime.mcall. But why? Who called it? Looking at remaining goroutine stacks, I see "goroutine 58 [runnable]" allocating memory at trace_test.go:149 with "_ = make([]byte, 1&lt;&lt;20)". But how did we get from allocating memory into runtime.mcall?</li>
</ul>
<p dir="auto">I suspect there is missing information here. Is it OK for it to be missing? How should I debug this crash?</p>
<p dir="auto">Perhaps I am misreading this altogether.</p>
<p dir="auto">Alex</p>
<p dir="auto">Not sure this is the same as <a class="issue-link js-issue-link" data-error-text="Failed to load title" data-id="58467559" data-permission-text="Title is private" data-url="https://github.com/golang/go/issues/9953" data-hovercard-type="issue" data-hovercard-url="/golang/go/issues/9953/hovercard" href="https://github.com/golang/go/issues/9953">#9953</a>.</p>
<div class="snippet-clipboard-content notranslate position-relative overflow-auto" data-snippet-clipboard-copy-content="fatal error: unexpected signal during runtime execution
[signal 0xa code=0xc addr=0x28316794 pc=0x80548be]

runtime stack:
runtime.throw(0x82311a8, 0x2a)
    /tmp/buildlet-scatch766897833/go/src/runtime/panic.go:543 +0x80
runtime.sigpanic()
    /tmp/buildlet-scatch766897833/go/src/runtime/sigpanic_unix.go:12 +0x54
runtime.gcmarkwb_m(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:73 +0xae
runtime.writebarrierptr_nostore1.func1()
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:111 +0x115
runtime.systemstack(0x38409e88)
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:283 +0x77
runtime.writebarrierptr_nostore1(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:112 +0x44
runtime.writebarrierptr(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:135 +0x7f
runtime.writebarrierslice(0x587a100c, 0x587a1218, 0x689d, 0xfde8)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:211 +0x1e
runtime.traceEvent(0x383d6a0e, 0xffffffff, 0x38409f70, 0x1, 0x1)
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:502 +0x5af
runtime.traceGoStart()
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:770 +0x81
runtime.execute(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1214 +0xd7
runtime.schedule()
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1418 +0x76
runtime.goschedImpl(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1530 +0xd1
runtime.gosched_m(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1538 +0x33
runtime.mcall(0x383fc52c)
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:210 +0x43

goroutine 66 [running, locked to thread]:
runtime.Gosched()
    /tmp/buildlet-scatch766897833/go/src/runtime/proc.go:135 +0x10 fp=0x4c2497d4 sp=0x4c2497cc
runtime/pprof_test.TestTraceStressStartStop.func1.5(0x383e6140)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:269 +0x4a fp=0x4c2497e8 sp=0x4c2497d4
runtime.goexit()
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:2431 +0x1 fp=0x4c2497ec sp=0x4c2497e8
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:272 +0x233

goroutine 1 [chan receive]:
testing.RunTests(0x82528e8, 0x82e7160, 0xe, 0xe, 0x1)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:561 +0x864
testing.(*M).Run(0x383e8120, 0x82fdac0)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:490 +0x65
main.main()
    /tmp/go-build720119124/runtime/pprof/_test/_testmain.go:82 +0x171

goroutine 89 [semacquire]:
runtime.StopTrace()
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:184 +0x28
runtime/pprof.StopTrace()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:642 +0x18
runtime/pprof_test.TestTraceStressStartStop(0x4c23a240)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:356 +0x1c0
testing.tRunner(0x4c23a240, 0x82e71f0)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:452 +0xa0
created by testing.RunTests
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:560 +0x832

goroutine 40 [select (no cases)]:
runtime/pprof_test.TestTraceSymbolize.func1()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:38 +0x18
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:39 +0x179

goroutine 41 [chan send (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func2()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:42 +0x38
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:43 +0x18e

goroutine 42 [chan receive (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func3()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:46 +0x30
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:47 +0x1a3

goroutine 90 [runnable]:
runtime/pprof_test.TestTraceStressStartStop.func1(0x384690c0, 0x4c23a240)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:277 +0x271
created by runtime/pprof_test.TestTraceStressStartStop
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:348 +0x99

goroutine 113 [chan receive]:
runtime/pprof_test.TestTraceStressStartStop.func1.2(0x383e6140, 0x4c23c020)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:241 +0x32
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:243 +0xb7

goroutine 114 [syscall]:
syscall.Syscall(0x3, 0x3ea03fcf, 0x1, 0x1, 0x0, 0x58751218, 0x3128)
    /tmp/buildlet-scatch766897833/go/src/syscall/asm_freebsd_386.s:20 +0x5
syscall.read(0x3, 0x3ea03fcf, 0x1, 0x1, 0xb23bb542, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/syscall/zsyscall_freebsd_386.go:890 +0x50
syscall.Read(0x3, 0x3ea03fcf, 0x1, 0x1, 0x58751000, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/syscall/syscall_unix.go:136 +0x46
os.(*File).read(0x4c23e000, 0x3ea03fcf, 0x1, 0x1, 0x9, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/os/file_unix.go:203 +0x6c
os.(*File).Read(0x4c23e000, 0x3ea03fcf, 0x1, 0x1, 0xfde8, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/os/file.go:95 +0x6c
runtime/pprof_test.TestTraceStressStartStop.func1.4(0x4c23e000, 0x383e6140, 0x4c23c020)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:256 +0x54
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:259 +0x202

goroutine 98 [select (no cases)]:
runtime/pprof_test.TestTraceStress.func9()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:205 +0x1d
created by runtime/pprof_test.TestTraceStress
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:206 +0x82c

goroutine 67 [trace reader (blocked)]:
runtime.ReadTrace(0x0, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:313 +0x1d2
runtime/pprof.StartTrace.func1(0x584e8918, 0x383eb440)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:629 +0x1b
created by runtime/pprof.StartTrace
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:635 +0x6a
FAIL    runtime/pprof   7.732s"><pre class="notranslate"><code class="notranslate">fatal error: unexpected signal during runtime execution
[signal 0xa code=0xc addr=0x28316794 pc=0x80548be]

runtime stack:
runtime.throw(0x82311a8, 0x2a)
    /tmp/buildlet-scatch766897833/go/src/runtime/panic.go:543 +0x80
runtime.sigpanic()
    /tmp/buildlet-scatch766897833/go/src/runtime/sigpanic_unix.go:12 +0x54
runtime.gcmarkwb_m(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:73 +0xae
runtime.writebarrierptr_nostore1.func1()
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:111 +0x115
runtime.systemstack(0x38409e88)
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:283 +0x77
runtime.writebarrierptr_nostore1(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:112 +0x44
runtime.writebarrierptr(0x587a100c, 0x587a1218)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:135 +0x7f
runtime.writebarrierslice(0x587a100c, 0x587a1218, 0x689d, 0xfde8)
    /tmp/buildlet-scatch766897833/go/src/runtime/mbarrier.go:211 +0x1e
runtime.traceEvent(0x383d6a0e, 0xffffffff, 0x38409f70, 0x1, 0x1)
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:502 +0x5af
runtime.traceGoStart()
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:770 +0x81
runtime.execute(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1214 +0xd7
runtime.schedule()
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1418 +0x76
runtime.goschedImpl(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1530 +0xd1
runtime.gosched_m(0x383d74a0)
    /tmp/buildlet-scatch766897833/go/src/runtime/proc1.go:1538 +0x33
runtime.mcall(0x383fc52c)
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:210 +0x43

goroutine 66 [running, locked to thread]:
runtime.Gosched()
    /tmp/buildlet-scatch766897833/go/src/runtime/proc.go:135 +0x10 fp=0x4c2497d4 sp=0x4c2497cc
runtime/pprof_test.TestTraceStressStartStop.func1.5(0x383e6140)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:269 +0x4a fp=0x4c2497e8 sp=0x4c2497d4
runtime.goexit()
    /tmp/buildlet-scatch766897833/go/src/runtime/asm_386.s:2431 +0x1 fp=0x4c2497ec sp=0x4c2497e8
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:272 +0x233

goroutine 1 [chan receive]:
testing.RunTests(0x82528e8, 0x82e7160, 0xe, 0xe, 0x1)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:561 +0x864
testing.(*M).Run(0x383e8120, 0x82fdac0)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:490 +0x65
main.main()
    /tmp/go-build720119124/runtime/pprof/_test/_testmain.go:82 +0x171

goroutine 89 [semacquire]:
runtime.StopTrace()
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:184 +0x28
runtime/pprof.StopTrace()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:642 +0x18
runtime/pprof_test.TestTraceStressStartStop(0x4c23a240)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:356 +0x1c0
testing.tRunner(0x4c23a240, 0x82e71f0)
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:452 +0xa0
created by testing.RunTests
    /tmp/buildlet-scatch766897833/go/src/testing/testing.go:560 +0x832

goroutine 40 [select (no cases)]:
runtime/pprof_test.TestTraceSymbolize.func1()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:38 +0x18
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:39 +0x179

goroutine 41 [chan send (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func2()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:42 +0x38
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:43 +0x18e

goroutine 42 [chan receive (nil chan)]:
runtime/pprof_test.TestTraceSymbolize.func3()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:46 +0x30
created by runtime/pprof_test.TestTraceSymbolize
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_stack_test.go:47 +0x1a3

goroutine 90 [runnable]:
runtime/pprof_test.TestTraceStressStartStop.func1(0x384690c0, 0x4c23a240)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:277 +0x271
created by runtime/pprof_test.TestTraceStressStartStop
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:348 +0x99

goroutine 113 [chan receive]:
runtime/pprof_test.TestTraceStressStartStop.func1.2(0x383e6140, 0x4c23c020)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:241 +0x32
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:243 +0xb7

goroutine 114 [syscall]:
syscall.Syscall(0x3, 0x3ea03fcf, 0x1, 0x1, 0x0, 0x58751218, 0x3128)
    /tmp/buildlet-scatch766897833/go/src/syscall/asm_freebsd_386.s:20 +0x5
syscall.read(0x3, 0x3ea03fcf, 0x1, 0x1, 0xb23bb542, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/syscall/zsyscall_freebsd_386.go:890 +0x50
syscall.Read(0x3, 0x3ea03fcf, 0x1, 0x1, 0x58751000, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/syscall/syscall_unix.go:136 +0x46
os.(*File).read(0x4c23e000, 0x3ea03fcf, 0x1, 0x1, 0x9, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/os/file_unix.go:203 +0x6c
os.(*File).Read(0x4c23e000, 0x3ea03fcf, 0x1, 0x1, 0xfde8, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/os/file.go:95 +0x6c
runtime/pprof_test.TestTraceStressStartStop.func1.4(0x4c23e000, 0x383e6140, 0x4c23c020)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:256 +0x54
created by runtime/pprof_test.TestTraceStressStartStop.func1
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:259 +0x202

goroutine 98 [select (no cases)]:
runtime/pprof_test.TestTraceStress.func9()
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:205 +0x1d
created by runtime/pprof_test.TestTraceStress
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/trace_test.go:206 +0x82c

goroutine 67 [trace reader (blocked)]:
runtime.ReadTrace(0x0, 0x0, 0x0)
    /tmp/buildlet-scatch766897833/go/src/runtime/trace.go:313 +0x1d2
runtime/pprof.StartTrace.func1(0x584e8918, 0x383eb440)
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:629 +0x1b
created by runtime/pprof.StartTrace
    /tmp/buildlet-scatch766897833/go/src/runtime/pprof/pprof.go:635 +0x6a
FAIL    runtime/pprof   7.732s
</code></pre></div>