OXIESEC PANEL
- Current Dir:
/
/
opt
/
golang
/
1.19.4
/
src
/
runtime
Server IP: 2a02:4780:11:1084:0:327f:3464:10
Upload:
Create Dir:
Name
Size
Modified
Perms
π
..
-
12/01/2022 06:13:58 PM
rwxr-xr-x
π
HACKING.md
15.29 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
Makefile
178 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
abi_test.go
2.83 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
alg.go
9.45 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
align_runtime_test.go
2.73 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
align_test.go
5.26 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asan
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
asan.go
1.55 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asan0.go
761 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
asan_amd64.s
2.46 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asan_arm64.s
2.15 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asan_riscv64.s
1.92 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm.s
278 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_386.s
40.43 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_amd64.h
411 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_amd64.s
57.44 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_arm.s
30.2 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_arm64.s
41.41 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_loong64.s
21.79 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_mips64x.s
22.43 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_mipsx.s
24.41 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_ppc64x.h
1023 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_ppc64x.s
35.21 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_riscv64.s
26.43 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_s390x.s
26.08 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
asm_wasm.s
9.38 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_arm64.s
259 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_loong64.s
245 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_mips64x.s
300 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_mipsx.s
262 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_pointer.go
2.62 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_ppc64x.s
437 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
atomic_riscv64.s
275 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
auxv_none.go
298 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
callers_test.go
8.44 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cgo
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
cgo.go
2 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cgo_mmap.go
2.4 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cgo_ppc64x.go
418 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
cgo_sigaction.go
3.28 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cgocall.go
19.12 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cgocallback.go
317 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
cgocheck.go
6.86 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
chan.go
23.73 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
chan_test.go
23.37 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
chanbarrier_test.go
1.4 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
checkptr.go
3.29 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
checkptr_test.go
2.73 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
closure_test.go
937 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
compiler.go
410 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
complex.go
1.59 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
complex_test.go
1.05 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
conv_wasm_test.go
2.96 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cpuflags.go
810 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
cpuflags_amd64.go
533 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
cpuflags_arm64.go
334 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
cpuprof.go
7.78 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
cputicks.go
449 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
crash_cgo_test.go
18.14 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
crash_test.go
21.77 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
crash_unix_test.go
8.39 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debug
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
debug.go
3.23 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debug_test.go
7.98 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debugcall.go
6.19 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debuglog.go
17.87 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debuglog_off.go
357 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
debuglog_on.go
1.09 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
debuglog_test.go
4.56 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defer_test.go
11.56 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_linux.go
845 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_netbsd_386.go
2.83 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_netbsd_amd64.go
3.06 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_netbsd_arm.go
2.94 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_netbsd_arm64.go
3.17 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs1_solaris_amd64.go
4 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs2_linux.go
3.51 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs3_linux.go
1.09 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_aix.go
4.16 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_aix_ppc64.go
3.61 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_arm_linux.go
2.67 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_darwin.go
3.78 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_darwin_amd64.go
6.07 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_darwin_arm64.go
3.89 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_dragonfly.go
2.59 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_dragonfly_amd64.go
3.29 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_freebsd.go
3.82 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_freebsd_386.go
4.36 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_freebsd_amd64.go
4.63 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_freebsd_arm.go
3.69 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_freebsd_arm64.go
4.01 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_illumos_amd64.go
285 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux.go
3.25 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_386.go
4.42 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_amd64.go
4.93 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_arm.go
4.11 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_arm64.go
3.86 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_loong64.go
3.68 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_mips64x.go
3.85 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_mipsx.go
3.83 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_ppc64.go
3.93 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_ppc64le.go
3.93 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_riscv64.go
4.06 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_linux_s390x.go
3.41 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_netbsd.go
2.72 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_netbsd_386.go
855 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_netbsd_amd64.go
1.01 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_netbsd_arm.go
764 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd.go
3.09 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd_386.go
2.87 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd_amd64.go
3.07 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd_arm.go
2.99 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd_arm64.go
2.74 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_openbsd_mips64.go
2.64 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_plan9_386.go
1.63 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_plan9_amd64.go
1.82 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_plan9_arm.go
1.73 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_solaris.go
3.31 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_solaris_amd64.go
1004 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_windows.go
2.09 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_windows_386.go
1.98 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_windows_amd64.go
2.71 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_windows_arm.go
2.11 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
defs_windows_arm64.go
2.63 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_386.s
8.24 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_amd64.s
5.62 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_arm.s
7.11 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_arm64.s
5.27 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_loong64.s
12 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_mips64x.s
11.28 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_ppc64x.s
7.06 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_riscv64.s
11.4 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
duff_s390x.s
507 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
env_plan9.go
3 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
env_posix.go
1.79 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
env_test.go
1.16 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
error.go
9.21 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
example_test.go
1.55 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_aix_test.go
234 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_arm_test.go
226 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_darwin_test.go
382 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_debug_amd64_test.go
3.6 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_debug_arm64_test.go
3.49 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_debug_test.go
5.05 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_debuglog_test.go
1.24 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_linux_test.go
550 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_mmap_test.go
429 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_pipe2_test.go
310 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_pipe_test.go
219 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_solaris_test.go
282 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
export_test.go
38.87 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_unix_test.go
2.18 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
export_windows_test.go
677 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
extern.go
13.62 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
fastlog2.go
1.22 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
fastlog2_test.go
784 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
fastlog2table.go
904 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
float.go
1.35 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
float_test.go
699 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
funcdata.h
2.55 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
gc_test.go
20.04 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
gcinfo_test.go
5.59 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
go_tls.h
366 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
hash32.go
1.58 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
hash64.go
1.95 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
hash_test.go
16.77 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
heapdump.go
17.65 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
histogram.go
6.19 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
histogram_test.go
3.42 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
iface.go
15.66 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
iface_test.go
7.45 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
internal
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
lfstack.go
1.77 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lfstack_32bit.go
532 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
lfstack_64bit.go
2.18 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lfstack_test.go
2.77 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
libfuzzer.go
6.5 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
libfuzzer_amd64.s
5.01 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
libfuzzer_arm64.s
3.15 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lock_futex.go
5.19 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lock_js.go
6.14 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lock_sema.go
6.74 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lockrank.go
13.26 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lockrank_off.go
1.14 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lockrank_on.go
9.83 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
lockrank_test.go
1.15 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
malloc.go
51.01 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
malloc_test.go
10.78 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map.go
43.52 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map_benchmark_test.go
10.48 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map_fast32.go
12.72 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map_fast64.go
12.91 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map_faststr.go
14.3 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
map_test.go
27.44 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mbarrier.go
12.43 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mbitmap.go
66.08 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mcache.go
10 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mcentral.go
7.9 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mcheckmark.go
2.81 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem.go
6.23 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_aix.go
1.9 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_bsd.go
2.03 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_darwin.go
1.84 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_js.go
2.25 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_linux.go
6.15 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_plan9.go
4.32 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mem_windows.go
3.76 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_386.s
2.38 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_amd64.s
4.91 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_arm.s
2.6 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_arm64.s
3.62 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_loong64.s
778 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_mips64x.s
1.72 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_mipsx.s
1.32 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_plan9_386.s
983 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_plan9_amd64.s
511 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_ppc64x.s
4.23 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_riscv64.s
978 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_s390x.s
1.96 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memclr_wasm.s
622 bytes
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_386.s
4.42 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_amd64.s
12.48 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_arm.s
5.9 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_arm64.s
5.96 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_linux_amd64_test.go
1.6 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_loong64.s
1.8 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_mips64x.s
1.83 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_mipsx.s
4.4 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_plan9_386.s
3.06 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_plan9_amd64.s
3.04 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_ppc64x.s
4.58 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_riscv64.s
1.86 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_s390x.s
2.92 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_test.go
14.03 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
memmove_wasm.s
1.74 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
metrics
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
metrics.go
18.71 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
metrics_test.go
14.74 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mfinal.go
16.34 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mfinal_test.go
6.19 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mfixalloc.go
3.07 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mgc.go
56.37 KB
12/01/2022 06:12:59 PM
rw-r--r--
π
mgclimit.go
17.26 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgclimit_test.go
9.02 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcmark.go
47.47 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcpacer.go
60.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcpacer_test.go
40.43 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcscavenge.go
41.29 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcscavenge_test.go
20.33 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcstack.go
10.58 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcsweep.go
27.89 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mgcwork.go
12.86 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mheap.go
69.14 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mkduff.go
8.01 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mkfastlog2table.go
3.08 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mkpreempt.go
15.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mksizeclasses.go
9.3 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mmap.go
821 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagealloc.go
36.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagealloc_32bit.go
3.81 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagealloc_64bit.go
9.44 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagealloc_test.go
32.59 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagecache.go
5.46 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpagecache_test.go
10.79 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpallocbits.go
12.6 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mpallocbits_test.go
13.69 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mprof.go
38.51 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mranges.go
13.64 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mranges_test.go
5.68 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
msan
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
msan.go
1.5 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
msan0.go
725 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
msan_amd64.s
2.31 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
msan_arm64.s
1.99 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
msize.go
777 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
mspanset.go
12.21 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mstats.go
30.07 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
mwbbuf.go
9.28 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_fcntl_libc_test.go
470 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_fcntl_unix_test.go
458 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_pipe.go
405 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_pipe2.go
344 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_pipe_test.go
706 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
nbpipe_test.go
1.68 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
net_plan9.go
645 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll.go
18.27 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_aix.go
4.83 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_epoll.go
4.16 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_fake.go
652 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_kqueue.go
4.56 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_os_test.go
360 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_solaris.go
10.76 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_stub.go
1.41 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
netpoll_windows.go
3.75 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
norace_linux_test.go
915 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
norace_test.go
983 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
numcpu_freebsd_test.go
381 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os2_aix.go
20.45 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os2_freebsd.go
302 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os2_openbsd.go
296 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os2_plan9.go
1.48 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os2_solaris.go
320 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os3_plan9.go
3.93 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os3_solaris.go
17.22 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_aix.go
8.61 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_android.go
463 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_darwin.go
12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_darwin_arm64.go
416 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_dragonfly.go
6.96 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd.go
11.61 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd2.go
603 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd_amd64.go
658 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd_arm.go
1.32 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd_arm64.go
398 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_freebsd_noauxv.go
241 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_illumos.go
3.93 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_js.go
3.28 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux.go
26.14 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_arm.go
1.35 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_arm64.go
556 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_be64.go
824 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_generic.go
888 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_loong64.go
485 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_mips64x.go
1.07 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_mipsx.go
1.06 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_noauxv.go
337 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_novdso.go
347 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_ppc64x.go
526 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_riscv64.go
198 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_s390x.go
316 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_linux_x86.go
234 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_netbsd.go
9.8 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_netbsd_386.go
617 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_netbsd_amd64.go
614 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_netbsd_arm.go
1.16 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_netbsd_arm64.go
856 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_nonopenbsd.go
437 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_only_solaris.go
357 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd.go
6.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_arm.go
749 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_arm64.go
416 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_libc.go
1.71 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_mips64.go
416 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_syscall.go
1.27 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_syscall1.go
441 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_openbsd_syscall2.go
2.46 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_plan9.go
10.3 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_plan9_arm.go
462 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_solaris.go
6.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_windows.go
44.43 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
os_windows_arm.go
511 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
os_windows_arm64.go
339 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
panic.go
40.25 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
panic32.go
4.8 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
panic_test.go
1.71 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
plugin.go
4.26 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
pprof
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
preempt.go
15.21 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_386.s
824 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_amd64.s
1.62 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_arm.s
1.48 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_arm64.s
1.97 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_loong64.s
2.35 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_mips64x.s
2.72 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_mipsx.s
2.68 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_nonwindows.go
290 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_ppc64x.s
2.72 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_riscv64.s
2.26 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_s390x.s
1.01 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
preempt_wasm.s
176 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
print.go
5.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
proc.go
176.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
proc_runtime_test.go
1.38 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
proc_test.go
25.66 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
profbuf.go
18.26 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
profbuf_test.go
8.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
proflabel.go
1.52 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
race.go
18.58 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race0.go
2.79 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race_amd64.s
13.82 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race_arm64.s
14.21 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race_ppc64le.s
17.89 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
race_s390x.s
12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rand_test.go
907 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rdebug.go
553 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
relax_stub.go
598 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_aix_ppc64.s
4.33 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_android_386.s
822 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_android_amd64.s
754 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_android_arm.s
843 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_android_arm64.s
941 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_darwin_amd64.s
399 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_darwin_arm64.s
1.69 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_dragonfly_amd64.s
448 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_freebsd_386.s
454 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_freebsd_amd64.s
442 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_freebsd_arm.s
298 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_freebsd_arm64.s
1.88 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_illumos_amd64.s
311 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_ios_amd64.s
425 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_ios_arm64.s
425 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_js_wasm.s
2.3 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_386.s
450 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_amd64.s
307 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_arm.s
1007 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_arm64.s
1.81 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_loong64.s
716 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_mips64x.s
1014 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_mipsx.s
797 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_ppc64.s
928 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_ppc64le.s
4.35 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_riscv64.s
2.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_linux_s390x.s
676 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_netbsd_386.s
452 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_netbsd_amd64.s
309 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_netbsd_arm.s
296 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_netbsd_arm64.s
1.8 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_openbsd_386.s
454 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_openbsd_amd64.s
311 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_openbsd_arm.s
298 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_openbsd_arm64.s
1.96 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_openbsd_mips64.s
976 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_plan9_386.s
523 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_plan9_amd64.s
481 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_plan9_arm.s
397 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_solaris_amd64.s
311 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_windows_386.s
1.28 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_windows_amd64.s
986 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_windows_arm.s
386 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
rt0_windows_arm64.s
725 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime-gdb.py
15.33 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime-gdb_test.go
20.93 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime-lldb_test.go
4.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime.go
1.45 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime1.go
13.06 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime2.go
43.07 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime_boring.go
606 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime_linux_test.go
1.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime_mmap_test.go
1.77 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime_test.go
11.79 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
runtime_unix_test.go
1.22 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rwmutex.go
3.53 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
rwmutex_test.go
4.19 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
select.go
14.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sema.go
16.16 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sema_test.go
4.21 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
semasleep_test.go
3.05 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigaction.go
489 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_386.go
1.72 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_aix_ppc64.go
3.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_amd64.go
2.73 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_arm.go
2.54 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_arm64.go
3.21 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_darwin.go
2.13 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_darwin_amd64.go
4 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_darwin_arm64.go
3.6 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_dragonfly.go
2.17 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_dragonfly_amd64.go
2.01 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_freebsd.go
2.2 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_freebsd_386.go
1.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_freebsd_amd64.go
2.03 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_freebsd_arm.go
2.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_freebsd_arm64.go
3.23 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_386.go
1.59 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_amd64.go
2.05 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_arm.go
2.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_arm64.go
2.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_loong64.go
3.22 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_mips64x.go
3.35 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_mipsx.go
3.67 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_ppc64x.go
3.42 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_riscv64.go
2.92 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_linux_s390x.go
4.49 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_loong64.go
3.09 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_mips64x.go
3.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_mipsx.go
3.06 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_netbsd.go
2.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_netbsd_386.go
1.76 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_netbsd_amd64.go
2.33 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_netbsd_arm.go
2.3 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_netbsd_arm64.go
3.4 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd.go
2.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd_386.go
1.58 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd_amd64.go
2.04 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd_arm.go
2.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd_arm64.go
3.38 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_openbsd_mips64.go
3.28 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_plan9.go
1.93 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_ppc64x.go
3.64 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_riscv64.go
2.89 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_solaris.go
4.5 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_solaris_amd64.go
2.47 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_unix.go
41.88 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_windows.go
9.27 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
signal_windows_test.go
5.29 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigqueue.go
7.66 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigqueue_note.go
648 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sigqueue_plan9.go
3.25 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigtab_aix.go
11.3 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigtab_linux_generic.go
3.52 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sigtab_linux_mipsx.go
5.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sizeclasses.go
9.14 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sizeof_test.go
893 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
slice.go
9.87 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
slice_test.go
10.32 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
softfloat64.go
11.54 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
softfloat64_test.go
4.04 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stack.go
45.05 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stack_test.go
22.39 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
string.go
13.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
string_test.go
12.61 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs.go
19.37 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs2.go
1.13 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs3.go
274 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_386.go
550 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_amd64.go
1.2 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_arm.go
531 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_arm64.go
555 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_linux.go
650 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_loong64.go
276 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_mips64x.go
364 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_mipsx.go
283 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_nonlinux.go
298 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_ppc64.go
301 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_ppc64x.go
453 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_riscv64.go
460 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
stubs_s390x.go
256 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
symtab.go
35.81 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
symtab_test.go
7.48 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_aix_ppc64.s
7.42 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_arm.go
521 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_arm64.go
469 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_darwin.go
17.92 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_darwin_amd64.s
19.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_darwin_arm64.go
1.74 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_darwin_arm64.s
15.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_dragonfly_amd64.s
8.03 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_freebsd_386.s
8.41 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_freebsd_amd64.s
10.7 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_freebsd_arm.s
10.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_freebsd_arm64.s
9.4 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_libc.go
1.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_386.s
18.31 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_amd64.s
16.57 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_arm.s
16.12 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_arm64.s
18.09 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_loong64.s
12.15 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_mips64x.s
13.5 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_mipsx.s
11.09 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_ppc64x.s
22.1 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_riscv64.s
12.59 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_linux_s390x.s
13.78 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_loong64.go
489 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_mips64x.go
500 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_mipsx.go
496 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_netbsd_386.s
9.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_netbsd_amd64.s
9.51 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_netbsd_arm.s
10.41 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_netbsd_arm64.s
9.38 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_nonppc64x.go
245 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd.go
2.59 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd1.go
1.23 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd2.go
8.36 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd3.go
3.37 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd_386.s
20.03 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd_amd64.s
16.64 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd_arm.s
18.15 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd_arm64.s
14.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_openbsd_mips64.s
8.6 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_plan9_386.s
4.48 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_plan9_amd64.s
4.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_plan9_arm.s
7.03 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_ppc64x.go
532 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_riscv64.go
469 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_s390x.go
469 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_solaris_amd64.s
6.42 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_wasm.go
754 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_wasm.s
2.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_windows_386.s
7.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_windows_amd64.s
8.88 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_windows_arm.s
11.97 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_windows_arm64.s
11.45 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
sys_x86.go
552 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
syscall2_solaris.go
1.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
syscall_aix.go
6 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
syscall_solaris.go
8.01 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
syscall_windows.go
16.95 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
syscall_windows_test.go
32.96 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
testdata
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
textflag.h
1.52 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time.go
30.75 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_fake.go
2.5 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_linux_amd64.s
2.02 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_nofake.go
709 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
time_test.go
2.03 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_windows.h
753 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
time_windows_386.s
1.79 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_windows_amd64.s
871 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
time_windows_arm.s
2.1 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
time_windows_arm64.s
1021 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
timeasm.go
418 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
timestub.go
532 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
timestub2.go
314 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_arm.s
3.45 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_arm64.h
1.1 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_arm64.s
1.2 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_loong64.s
589 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_mips64x.s
733 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_mipsx.s
709 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_ppc64x.s
1.5 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_riscv64.s
726 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_s390x.s
1.55 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_stub.go
260 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
tls_windows_amd64.go
294 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
trace
-
12/01/2022 06:13:56 PM
rwxr-xr-x
π
trace.go
45.8 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
traceback.go
48.18 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
traceback_test.go
11.64 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
type.go
17.43 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
typekind.go
742 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
utf8.go
3.39 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_elf32.go
2.76 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_elf64.go
2.84 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_freebsd.go
2.44 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_freebsd_arm.go
454 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_freebsd_arm64.go
443 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_freebsd_x86.go
1.85 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_in_none.go
443 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux.go
7.77 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_386.go
669 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_amd64.go
685 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_arm.go
669 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_arm64.go
670 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_loong64.go
793 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_mips64x.go
850 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_ppc64x.go
672 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_riscv64.go
666 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vdso_linux_s390x.go
681 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
vlop_386.s
2.02 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vlop_arm.s
7.06 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vlop_arm_test.go
3.75 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
vlrt.go
6.71 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
wincallback.go
3.45 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
write_err.go
291 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
write_err_android.go
4.65 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
zcallback_windows.go
155 bytes
12/01/2022 06:13:00 PM
rw-r--r--
π
zcallback_windows.s
63.02 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
zcallback_windows_arm.s
89.32 KB
12/01/2022 06:13:00 PM
rw-r--r--
π
zcallback_windows_arm64.s
89.32 KB
12/01/2022 06:13:00 PM
rw-r--r--
Editing: select.go
Close
// Copyright 2009 The Go Authors. All rights reserved. // Use of this source code is governed by a BSD-style // license that can be found in the LICENSE file. package runtime // This file contains the implementation of Go select statements. import ( "internal/abi" "runtime/internal/atomic" "unsafe" ) const debugSelect = false // Select case descriptor. // Known to compiler. // Changes here must also be made in src/cmd/compile/internal/walk/select.go's scasetype. type scase struct { c *hchan // chan elem unsafe.Pointer // data element } var ( chansendpc = abi.FuncPCABIInternal(chansend) chanrecvpc = abi.FuncPCABIInternal(chanrecv) ) func selectsetpc(pc *uintptr) { *pc = getcallerpc() } func sellock(scases []scase, lockorder []uint16) { var c *hchan for _, o := range lockorder { c0 := scases[o].c if c0 != c { c = c0 lock(&c.lock) } } } func selunlock(scases []scase, lockorder []uint16) { // We must be very careful here to not touch sel after we have unlocked // the last lock, because sel can be freed right after the last unlock. // Consider the following situation. // First M calls runtimeΒ·park() in runtimeΒ·selectgo() passing the sel. // Once runtimeΒ·park() has unlocked the last lock, another M makes // the G that calls select runnable again and schedules it for execution. // When the G runs on another M, it locks all the locks and frees sel. // Now if the first M touches sel, it will access freed memory. for i := len(lockorder) - 1; i >= 0; i-- { c := scases[lockorder[i]].c if i > 0 && c == scases[lockorder[i-1]].c { continue // will unlock it on the next iteration } unlock(&c.lock) } } func selparkcommit(gp *g, _ unsafe.Pointer) bool { // There are unlocked sudogs that point into gp's stack. Stack // copying must lock the channels of those sudogs. // Set activeStackChans here instead of before we try parking // because we could self-deadlock in stack growth on a // channel lock. gp.activeStackChans = true // Mark that it's safe for stack shrinking to occur now, // because any thread acquiring this G's stack for shrinking // is guaranteed to observe activeStackChans after this store. atomic.Store8(&gp.parkingOnChan, 0) // Make sure we unlock after setting activeStackChans and // unsetting parkingOnChan. The moment we unlock any of the // channel locks we risk gp getting readied by a channel operation // and so gp could continue running before everything before the // unlock is visible (even to gp itself). // This must not access gp's stack (see gopark). In // particular, it must not access the *hselect. That's okay, // because by the time this is called, gp.waiting has all // channels in lock order. var lastc *hchan for sg := gp.waiting; sg != nil; sg = sg.waitlink { if sg.c != lastc && lastc != nil { // As soon as we unlock the channel, fields in // any sudog with that channel may change, // including c and waitlink. Since multiple // sudogs may have the same channel, we unlock // only after we've passed the last instance // of a channel. unlock(&lastc.lock) } lastc = sg.c } if lastc != nil { unlock(&lastc.lock) } return true } func block() { gopark(nil, nil, waitReasonSelectNoCases, traceEvGoStop, 1) // forever } // selectgo implements the select statement. // // cas0 points to an array of type [ncases]scase, and order0 points to // an array of type [2*ncases]uint16 where ncases must be <= 65536. // Both reside on the goroutine's stack (regardless of any escaping in // selectgo). // // For race detector builds, pc0 points to an array of type // [ncases]uintptr (also on the stack); for other builds, it's set to // nil. // // selectgo returns the index of the chosen scase, which matches the // ordinal position of its respective select{recv,send,default} call. // Also, if the chosen scase was a receive operation, it reports whether // a value was received. func selectgo(cas0 *scase, order0 *uint16, pc0 *uintptr, nsends, nrecvs int, block bool) (int, bool) { if debugSelect { print("select: cas0=", cas0, "\n") } // NOTE: In order to maintain a lean stack size, the number of scases // is capped at 65536. cas1 := (*[1 << 16]scase)(unsafe.Pointer(cas0)) order1 := (*[1 << 17]uint16)(unsafe.Pointer(order0)) ncases := nsends + nrecvs scases := cas1[:ncases:ncases] pollorder := order1[:ncases:ncases] lockorder := order1[ncases:][:ncases:ncases] // NOTE: pollorder/lockorder's underlying array was not zero-initialized by compiler. // Even when raceenabled is true, there might be select // statements in packages compiled without -race (e.g., // ensureSigM in runtime/signal_unix.go). var pcs []uintptr if raceenabled && pc0 != nil { pc1 := (*[1 << 16]uintptr)(unsafe.Pointer(pc0)) pcs = pc1[:ncases:ncases] } casePC := func(casi int) uintptr { if pcs == nil { return 0 } return pcs[casi] } var t0 int64 if blockprofilerate > 0 { t0 = cputicks() } // The compiler rewrites selects that statically have // only 0 or 1 cases plus default into simpler constructs. // The only way we can end up with such small sel.ncase // values here is for a larger select in which most channels // have been nilled out. The general code handles those // cases correctly, and they are rare enough not to bother // optimizing (and needing to test). // generate permuted order norder := 0 for i := range scases { cas := &scases[i] // Omit cases without channels from the poll and lock orders. if cas.c == nil { cas.elem = nil // allow GC continue } j := fastrandn(uint32(norder + 1)) pollorder[norder] = pollorder[j] pollorder[j] = uint16(i) norder++ } pollorder = pollorder[:norder] lockorder = lockorder[:norder] // sort the cases by Hchan address to get the locking order. // simple heap sort, to guarantee n log n time and constant stack footprint. for i := range lockorder { j := i // Start with the pollorder to permute cases on the same channel. c := scases[pollorder[i]].c for j > 0 && scases[lockorder[(j-1)/2]].c.sortkey() < c.sortkey() { k := (j - 1) / 2 lockorder[j] = lockorder[k] j = k } lockorder[j] = pollorder[i] } for i := len(lockorder) - 1; i >= 0; i-- { o := lockorder[i] c := scases[o].c lockorder[i] = lockorder[0] j := 0 for { k := j*2 + 1 if k >= i { break } if k+1 < i && scases[lockorder[k]].c.sortkey() < scases[lockorder[k+1]].c.sortkey() { k++ } if c.sortkey() < scases[lockorder[k]].c.sortkey() { lockorder[j] = lockorder[k] j = k continue } break } lockorder[j] = o } if debugSelect { for i := 0; i+1 < len(lockorder); i++ { if scases[lockorder[i]].c.sortkey() > scases[lockorder[i+1]].c.sortkey() { print("i=", i, " x=", lockorder[i], " y=", lockorder[i+1], "\n") throw("select: broken sort") } } } // lock all the channels involved in the select sellock(scases, lockorder) var ( gp *g sg *sudog c *hchan k *scase sglist *sudog sgnext *sudog qp unsafe.Pointer nextp **sudog ) // pass 1 - look for something already waiting var casi int var cas *scase var caseSuccess bool var caseReleaseTime int64 = -1 var recvOK bool for _, casei := range pollorder { casi = int(casei) cas = &scases[casi] c = cas.c if casi >= nsends { sg = c.sendq.dequeue() if sg != nil { goto recv } if c.qcount > 0 { goto bufrecv } if c.closed != 0 { goto rclose } } else { if raceenabled { racereadpc(c.raceaddr(), casePC(casi), chansendpc) } if c.closed != 0 { goto sclose } sg = c.recvq.dequeue() if sg != nil { goto send } if c.qcount < c.dataqsiz { goto bufsend } } } if !block { selunlock(scases, lockorder) casi = -1 goto retc } // pass 2 - enqueue on all chans gp = getg() if gp.waiting != nil { throw("gp.waiting != nil") } nextp = &gp.waiting for _, casei := range lockorder { casi = int(casei) cas = &scases[casi] c = cas.c sg := acquireSudog() sg.g = gp sg.isSelect = true // No stack splits between assigning elem and enqueuing // sg on gp.waiting where copystack can find it. sg.elem = cas.elem sg.releasetime = 0 if t0 != 0 { sg.releasetime = -1 } sg.c = c // Construct waiting list in lock order. *nextp = sg nextp = &sg.waitlink if casi < nsends { c.sendq.enqueue(sg) } else { c.recvq.enqueue(sg) } } // wait for someone to wake us up gp.param = nil // Signal to anyone trying to shrink our stack that we're about // to park on a channel. The window between when this G's status // changes and when we set gp.activeStackChans is not safe for // stack shrinking. atomic.Store8(&gp.parkingOnChan, 1) gopark(selparkcommit, nil, waitReasonSelect, traceEvGoBlockSelect, 1) gp.activeStackChans = false sellock(scases, lockorder) gp.selectDone = 0 sg = (*sudog)(gp.param) gp.param = nil // pass 3 - dequeue from unsuccessful chans // otherwise they stack up on quiet channels // record the successful case, if any. // We singly-linked up the SudoGs in lock order. casi = -1 cas = nil caseSuccess = false sglist = gp.waiting // Clear all elem before unlinking from gp.waiting. for sg1 := gp.waiting; sg1 != nil; sg1 = sg1.waitlink { sg1.isSelect = false sg1.elem = nil sg1.c = nil } gp.waiting = nil for _, casei := range lockorder { k = &scases[casei] if sg == sglist { // sg has already been dequeued by the G that woke us up. casi = int(casei) cas = k caseSuccess = sglist.success if sglist.releasetime > 0 { caseReleaseTime = sglist.releasetime } } else { c = k.c if int(casei) < nsends { c.sendq.dequeueSudoG(sglist) } else { c.recvq.dequeueSudoG(sglist) } } sgnext = sglist.waitlink sglist.waitlink = nil releaseSudog(sglist) sglist = sgnext } if cas == nil { throw("selectgo: bad wakeup") } c = cas.c if debugSelect { print("wait-return: cas0=", cas0, " c=", c, " cas=", cas, " send=", casi < nsends, "\n") } if casi < nsends { if !caseSuccess { goto sclose } } else { recvOK = caseSuccess } if raceenabled { if casi < nsends { raceReadObjectPC(c.elemtype, cas.elem, casePC(casi), chansendpc) } else if cas.elem != nil { raceWriteObjectPC(c.elemtype, cas.elem, casePC(casi), chanrecvpc) } } if msanenabled { if casi < nsends { msanread(cas.elem, c.elemtype.size) } else if cas.elem != nil { msanwrite(cas.elem, c.elemtype.size) } } if asanenabled { if casi < nsends { asanread(cas.elem, c.elemtype.size) } else if cas.elem != nil { asanwrite(cas.elem, c.elemtype.size) } } selunlock(scases, lockorder) goto retc bufrecv: // can receive from buffer if raceenabled { if cas.elem != nil { raceWriteObjectPC(c.elemtype, cas.elem, casePC(casi), chanrecvpc) } racenotify(c, c.recvx, nil) } if msanenabled && cas.elem != nil { msanwrite(cas.elem, c.elemtype.size) } if asanenabled && cas.elem != nil { asanwrite(cas.elem, c.elemtype.size) } recvOK = true qp = chanbuf(c, c.recvx) if cas.elem != nil { typedmemmove(c.elemtype, cas.elem, qp) } typedmemclr(c.elemtype, qp) c.recvx++ if c.recvx == c.dataqsiz { c.recvx = 0 } c.qcount-- selunlock(scases, lockorder) goto retc bufsend: // can send to buffer if raceenabled { racenotify(c, c.sendx, nil) raceReadObjectPC(c.elemtype, cas.elem, casePC(casi), chansendpc) } if msanenabled { msanread(cas.elem, c.elemtype.size) } if asanenabled { asanread(cas.elem, c.elemtype.size) } typedmemmove(c.elemtype, chanbuf(c, c.sendx), cas.elem) c.sendx++ if c.sendx == c.dataqsiz { c.sendx = 0 } c.qcount++ selunlock(scases, lockorder) goto retc recv: // can receive from sleeping sender (sg) recv(c, sg, cas.elem, func() { selunlock(scases, lockorder) }, 2) if debugSelect { print("syncrecv: cas0=", cas0, " c=", c, "\n") } recvOK = true goto retc rclose: // read at end of closed channel selunlock(scases, lockorder) recvOK = false if cas.elem != nil { typedmemclr(c.elemtype, cas.elem) } if raceenabled { raceacquire(c.raceaddr()) } goto retc send: // can send to a sleeping receiver (sg) if raceenabled { raceReadObjectPC(c.elemtype, cas.elem, casePC(casi), chansendpc) } if msanenabled { msanread(cas.elem, c.elemtype.size) } if asanenabled { asanread(cas.elem, c.elemtype.size) } send(c, sg, cas.elem, func() { selunlock(scases, lockorder) }, 2) if debugSelect { print("syncsend: cas0=", cas0, " c=", c, "\n") } goto retc retc: if caseReleaseTime > 0 { blockevent(caseReleaseTime-t0, 1) } return casi, recvOK sclose: // send on closed channel selunlock(scases, lockorder) panic(plainError("send on closed channel")) } func (c *hchan) sortkey() uintptr { return uintptr(unsafe.Pointer(c)) } // A runtimeSelect is a single case passed to rselect. // This must match ../reflect/value.go:/runtimeSelect type runtimeSelect struct { dir selectDir typ unsafe.Pointer // channel type (not used here) ch *hchan // channel val unsafe.Pointer // ptr to data (SendDir) or ptr to receive buffer (RecvDir) } // These values must match ../reflect/value.go:/SelectDir. type selectDir int const ( _ selectDir = iota selectSend // case Chan <- Send selectRecv // case <-Chan: selectDefault // default ) //go:linkname reflect_rselect reflect.rselect func reflect_rselect(cases []runtimeSelect) (int, bool) { if len(cases) == 0 { block() } sel := make([]scase, len(cases)) orig := make([]int, len(cases)) nsends, nrecvs := 0, 0 dflt := -1 for i, rc := range cases { var j int switch rc.dir { case selectDefault: dflt = i continue case selectSend: j = nsends nsends++ case selectRecv: nrecvs++ j = len(cases) - nrecvs } sel[j] = scase{c: rc.ch, elem: rc.val} orig[j] = i } // Only a default case. if nsends+nrecvs == 0 { return dflt, false } // Compact sel and orig if necessary. if nsends+nrecvs < len(cases) { copy(sel[nsends:], sel[len(cases)-nrecvs:]) copy(orig[nsends:], orig[len(cases)-nrecvs:]) } order := make([]uint16, 2*(nsends+nrecvs)) var pc0 *uintptr if raceenabled { pcs := make([]uintptr, nsends+nrecvs) for i := range pcs { selectsetpc(&pcs[i]) } pc0 = &pcs[0] } chosen, recvOK := selectgo(&sel[0], &order[0], pc0, nsends, nrecvs, dflt == -1) // Translate chosen back to caller's ordering. if chosen < 0 { chosen = dflt } else { chosen = orig[chosen] } return chosen, recvOK } func (q *waitq) dequeueSudoG(sgp *sudog) { x := sgp.prev y := sgp.next if x != nil { if y != nil { // middle of queue x.next = y y.prev = x sgp.next = nil sgp.prev = nil return } // end of queue x.next = nil q.last = x sgp.prev = nil return } if y != nil { // start of queue y.prev = nil q.first = y sgp.next = nil return } // x==y==nil. Either sgp is the only element in the queue, // or it has already been removed. Use q.first to disambiguate. if q.first == sgp { q.first = nil q.last = nil } }