X7ROOT File Manager
Current Path:
/opt/golang/1.17.2/src/runtime
opt
/
golang
/
1.17.2
/
src
/
runtime
/
๐
..
๐
HACKING.md
(13.07 KB)
๐
Makefile
(178 B)
๐
abi_test.go
(2.88 KB)
๐
alg.go
(9.45 KB)
๐
asm.s
(715 B)
๐
asm_386.s
(40.27 KB)
๐
asm_amd64.s
(56.93 KB)
๐
asm_arm.s
(30.23 KB)
๐
asm_arm64.s
(33 KB)
๐
asm_mips64x.s
(22.43 KB)
๐
asm_mipsx.s
(24.39 KB)
๐
asm_ppc64x.h
(1023 B)
๐
asm_ppc64x.s
(29.16 KB)
๐
asm_riscv64.s
(22.43 KB)
๐
asm_s390x.s
(26.04 KB)
๐
asm_wasm.s
(9.8 KB)
๐
atomic_arm64.s
(259 B)
๐
atomic_mips64x.s
(326 B)
๐
atomic_mipsx.s
(284 B)
๐
atomic_pointer.go
(2.62 KB)
๐
atomic_ppc64x.s
(461 B)
๐
atomic_riscv64.s
(275 B)
๐
auxv_none.go
(360 B)
๐
callers_test.go
(7.72 KB)
๐
cgo
๐
cgo.go
(2.01 KB)
๐
cgo_mmap.go
(2.42 KB)
๐
cgo_ppc64x.go
(439 B)
๐
cgo_sigaction.go
(3.17 KB)
๐
cgocall.go
(18.88 KB)
๐
cgocallback.go
(317 B)
๐
cgocheck.go
(6.83 KB)
๐
chan.go
(23.54 KB)
๐
chan_test.go
(23.01 KB)
๐
chanbarrier_test.go
(1.4 KB)
๐
checkptr.go
(3.29 KB)
๐
checkptr_test.go
(1.62 KB)
๐
closure_test.go
(937 B)
๐
compiler.go
(413 B)
๐
complex.go
(1.59 KB)
๐
complex_test.go
(1.05 KB)
๐
conv_wasm_test.go
(2.96 KB)
๐
cpuflags.go
(800 B)
๐
cpuflags_amd64.go
(533 B)
๐
cpuflags_arm64.go
(334 B)
๐
cpuprof.go
(6.92 KB)
๐
cputicks.go
(497 B)
๐
crash_cgo_test.go
(16.17 KB)
๐
crash_nonunix_test.go
(429 B)
๐
crash_test.go
(20.96 KB)
๐
crash_unix_test.go
(8.52 KB)
๐
debug
๐
debug.go
(1.63 KB)
๐
debug_test.go
(6.82 KB)
๐
debugcall.go
(6.21 KB)
๐
debuglog.go
(17.49 KB)
๐
debuglog_off.go
(377 B)
๐
debuglog_on.go
(1.11 KB)
๐
debuglog_test.go
(4.56 KB)
๐
defer_test.go
(10.32 KB)
๐
defs1_linux.go
(862 B)
๐
defs1_netbsd_386.go
(2.84 KB)
๐
defs1_netbsd_amd64.go
(3.07 KB)
๐
defs1_netbsd_arm.go
(2.96 KB)
๐
defs1_netbsd_arm64.go
(3.18 KB)
๐
defs1_solaris_amd64.go
(4.02 KB)
๐
defs2_linux.go
(3.52 KB)
๐
defs3_linux.go
(1.11 KB)
๐
defs_aix.go
(4.18 KB)
๐
defs_aix_ppc64.go
(3.63 KB)
๐
defs_arm_linux.go
(2.69 KB)
๐
defs_darwin.go
(3.79 KB)
๐
defs_darwin_amd64.go
(6.07 KB)
๐
defs_darwin_arm64.go
(3.89 KB)
๐
defs_dragonfly.go
(2.63 KB)
๐
defs_dragonfly_amd64.go
(3.31 KB)
๐
defs_freebsd.go
(3.86 KB)
๐
defs_freebsd_386.go
(4.38 KB)
๐
defs_freebsd_amd64.go
(4.65 KB)
๐
defs_freebsd_arm.go
(3.71 KB)
๐
defs_freebsd_arm64.go
(4.03 KB)
๐
defs_illumos_amd64.go
(285 B)
๐
defs_linux.go
(3.05 KB)
๐
defs_linux_386.go
(3.77 KB)
๐
defs_linux_amd64.go
(4.28 KB)
๐
defs_linux_arm.go
(3.45 KB)
๐
defs_linux_arm64.go
(3.21 KB)
๐
defs_linux_mips64x.go
(3.24 KB)
๐
defs_linux_mipsx.go
(3.21 KB)
๐
defs_linux_ppc64.go
(3.28 KB)
๐
defs_linux_ppc64le.go
(3.28 KB)
๐
defs_linux_riscv64.go
(3.27 KB)
๐
defs_linux_s390x.go
(2.76 KB)
๐
defs_netbsd.go
(2.76 KB)
๐
defs_netbsd_386.go
(872 B)
๐
defs_netbsd_amd64.go
(1.03 KB)
๐
defs_netbsd_arm.go
(781 B)
๐
defs_openbsd.go
(3.1 KB)
๐
defs_openbsd_386.go
(2.89 KB)
๐
defs_openbsd_amd64.go
(3.09 KB)
๐
defs_openbsd_arm.go
(3 KB)
๐
defs_openbsd_arm64.go
(2.76 KB)
๐
defs_openbsd_mips64.go
(2.66 KB)
๐
defs_plan9_386.go
(1.63 KB)
๐
defs_plan9_amd64.go
(1.82 KB)
๐
defs_plan9_arm.go
(1.73 KB)
๐
defs_solaris.go
(3.35 KB)
๐
defs_solaris_amd64.go
(1021 B)
๐
defs_windows.go
(2.09 KB)
๐
defs_windows_386.go
(1.98 KB)
๐
defs_windows_amd64.go
(2.71 KB)
๐
defs_windows_arm.go
(2.11 KB)
๐
defs_windows_arm64.go
(2.63 KB)
๐
duff_386.s
(8.24 KB)
๐
duff_amd64.s
(5.62 KB)
๐
duff_arm.s
(7.11 KB)
๐
duff_arm64.s
(5.25 KB)
๐
duff_mips64x.s
(11.31 KB)
๐
duff_ppc64x.s
(2.43 KB)
๐
duff_riscv64.s
(11.38 KB)
๐
duff_s390x.s
(507 B)
๐
env_plan9.go
(2.99 KB)
๐
env_posix.go
(1.95 KB)
๐
env_test.go
(1.16 KB)
๐
error.go
(9.23 KB)
๐
example_test.go
(1.55 KB)
๐
export_aix_test.go
(204 B)
๐
export_arm_test.go
(226 B)
๐
export_darwin_test.go
(351 B)
๐
export_debug_regabiargs_off_test.go
(416 B)
๐
export_debug_regabiargs_on_test.go
(1.39 KB)
๐
export_debug_test.go
(5.86 KB)
๐
export_debuglog_test.go
(1.27 KB)
๐
export_futex_test.go
(570 B)
๐
export_linux_test.go
(429 B)
๐
export_mmap_test.go
(571 B)
๐
export_pipe2_test.go
(436 B)
๐
export_pipe_test.go
(240 B)
๐
export_solaris_test.go
(282 B)
๐
export_test.go
(30.12 KB)
๐
export_unix_test.go
(2.35 KB)
๐
export_windows_test.go
(652 B)
๐
extern.go
(12.58 KB)
๐
fastlog2.go
(1.22 KB)
๐
fastlog2_test.go
(784 B)
๐
fastlog2table.go
(904 B)
๐
float.go
(1.35 KB)
๐
funcdata.h
(2.47 KB)
๐
futex_test.go
(2.15 KB)
๐
gc_test.go
(19.21 KB)
๐
gcinfo_test.go
(5.69 KB)
๐
go_tls.h
(366 B)
๐
hash32.go
(1.61 KB)
๐
hash64.go
(2.01 KB)
๐
hash_test.go
(16.5 KB)
๐
heapdump.go
(17.74 KB)
๐
histogram.go
(6.42 KB)
๐
histogram_test.go
(1.85 KB)
๐
iface.go
(16.13 KB)
๐
iface_test.go
(7.51 KB)
๐
internal
๐
lfstack.go
(1.77 KB)
๐
lfstack_32bit.go
(562 B)
๐
lfstack_64bit.go
(2.24 KB)
๐
lfstack_test.go
(2.78 KB)
๐
libfuzzer.go
(2.6 KB)
๐
libfuzzer_amd64.s
(961 B)
๐
libfuzzer_arm64.s
(772 B)
๐
lock_futex.go
(5.22 KB)
๐
lock_js.go
(5.81 KB)
๐
lock_sema.go
(6.8 KB)
๐
lockrank.go
(11.62 KB)
๐
lockrank_off.go
(1.17 KB)
๐
lockrank_on.go
(9.84 KB)
๐
lockrank_test.go
(1.15 KB)
๐
malloc.go
(52.33 KB)
๐
malloc_test.go
(10.83 KB)
๐
map.go
(42.47 KB)
๐
map_benchmark_test.go
(10.51 KB)
๐
map_fast32.go
(12.63 KB)
๐
map_fast64.go
(12.82 KB)
๐
map_faststr.go
(14.15 KB)
๐
map_test.go
(27.52 KB)
๐
mbarrier.go
(12.2 KB)
๐
mbitmap.go
(65.27 KB)
๐
mcache.go
(9.68 KB)
๐
mcentral.go
(7.8 KB)
๐
mcheckmark.go
(2.81 KB)
๐
mem_aix.go
(1.94 KB)
๐
mem_bsd.go
(2.12 KB)
๐
mem_darwin.go
(1.88 KB)
๐
mem_js.go
(2.35 KB)
๐
mem_linux.go
(5.59 KB)
๐
mem_plan9.go
(4.53 KB)
๐
mem_windows.go
(3.87 KB)
๐
memclr_386.s
(2.42 KB)
๐
memclr_amd64.s
(3.89 KB)
๐
memclr_arm.s
(2.6 KB)
๐
memclr_arm64.s
(3.65 KB)
๐
memclr_mips64x.s
(1.75 KB)
๐
memclr_mipsx.s
(1.35 KB)
๐
memclr_plan9_386.s
(983 B)
๐
memclr_plan9_amd64.s
(511 B)
๐
memclr_ppc64x.s
(4.31 KB)
๐
memclr_riscv64.s
(926 B)
๐
memclr_s390x.s
(1.96 KB)
๐
memclr_wasm.s
(622 B)
๐
memmove_386.s
(4.46 KB)
๐
memmove_amd64.s
(12.66 KB)
๐
memmove_arm.s
(5.9 KB)
๐
memmove_arm64.s
(6 KB)
๐
memmove_linux_amd64_test.go
(1.6 KB)
๐
memmove_mips64x.s
(1.85 KB)
๐
memmove_mipsx.s
(4.42 KB)
๐
memmove_plan9_386.s
(3.06 KB)
๐
memmove_plan9_amd64.s
(3.04 KB)
๐
memmove_ppc64x.s
(4.11 KB)
๐
memmove_riscv64.s
(1.81 KB)
๐
memmove_s390x.s
(2.92 KB)
๐
memmove_test.go
(12.04 KB)
๐
memmove_wasm.s
(1.74 KB)
๐
metrics
๐
metrics.go
(17.69 KB)
๐
metrics_test.go
(12.48 KB)
๐
mfinal.go
(15.76 KB)
๐
mfinal_test.go
(5.85 KB)
๐
mfixalloc.go
(2.73 KB)
๐
mgc.go
(55.18 KB)
๐
mgcmark.go
(45.54 KB)
๐
mgcpacer.go
(29.56 KB)
๐
mgcscavenge.go
(35.05 KB)
๐
mgcscavenge_test.go
(12.74 KB)
๐
mgcstack.go
(10.58 KB)
๐
mgcsweep.go
(23.56 KB)
๐
mgcwork.go
(12.82 KB)
๐
mheap.go
(66.31 KB)
๐
mkduff.go
(7.19 KB)
๐
mkfastlog2table.go
(1.32 KB)
๐
mkpreempt.go
(14.17 KB)
๐
mksizeclasses.go
(9.31 KB)
๐
mmap.go
(990 B)
๐
mpagealloc.go
(36.77 KB)
๐
mpagealloc_32bit.go
(3.81 KB)
๐
mpagealloc_64bit.go
(6.65 KB)
๐
mpagealloc_test.go
(32.38 KB)
๐
mpagecache.go
(5.28 KB)
๐
mpagecache_test.go
(9.93 KB)
๐
mpallocbits.go
(12.01 KB)
๐
mpallocbits_test.go
(13.69 KB)
๐
mprof.go
(25.82 KB)
๐
mranges.go
(11.84 KB)
๐
mranges_test.go
(5.68 KB)
๐
msan
๐
msan.go
(1.51 KB)
๐
msan0.go
(741 B)
๐
msan_amd64.s
(2.32 KB)
๐
msan_arm64.s
(2.01 KB)
๐
msize.go
(777 B)
๐
mspanset.go
(12.2 KB)
๐
mstats.go
(30.65 KB)
๐
mwbbuf.go
(9.3 KB)
๐
nbpipe_fcntl_libc_test.go
(499 B)
๐
nbpipe_fcntl_unix_test.go
(507 B)
๐
nbpipe_pipe.go
(426 B)
๐
nbpipe_pipe2.go
(592 B)
๐
nbpipe_test.go
(2.26 KB)
๐
net_plan9.go
(645 B)
๐
netpoll.go
(16.24 KB)
๐
netpoll_aix.go
(4.87 KB)
๐
netpoll_epoll.go
(4.21 KB)
๐
netpoll_fake.go
(670 B)
๐
netpoll_kqueue.go
(4.64 KB)
๐
netpoll_os_test.go
(360 B)
๐
netpoll_solaris.go
(10.75 KB)
๐
netpoll_stub.go
(1.42 KB)
๐
netpoll_windows.go
(3.75 KB)
๐
norace_linux_test.go
(905 B)
๐
norace_test.go
(996 B)
๐
numcpu_freebsd_test.go
(381 B)
๐
os2_aix.go
(20.45 KB)
๐
os2_freebsd.go
(302 B)
๐
os2_openbsd.go
(296 B)
๐
os2_plan9.go
(1.48 KB)
๐
os2_solaris.go
(320 B)
๐
os3_plan9.go
(3.88 KB)
๐
os3_solaris.go
(17.02 KB)
๐
os_aix.go
(8.06 KB)
๐
os_android.go
(463 B)
๐
os_darwin.go
(11.54 KB)
๐
os_darwin_arm64.go
(416 B)
๐
os_dragonfly.go
(6.46 KB)
๐
os_freebsd.go
(11.2 KB)
๐
os_freebsd2.go
(507 B)
๐
os_freebsd_amd64.go
(529 B)
๐
os_freebsd_arm.go
(1.32 KB)
๐
os_freebsd_arm64.go
(398 B)
๐
os_freebsd_noauxv.go
(264 B)
๐
os_illumos.go
(3.93 KB)
๐
os_js.go
(3.26 KB)
๐
os_linux.go
(13.47 KB)
๐
os_linux_arm.go
(1.35 KB)
๐
os_linux_arm64.go
(572 B)
๐
os_linux_be64.go
(862 B)
๐
os_linux_generic.go
(950 B)
๐
os_linux_mips64x.go
(1.11 KB)
๐
os_linux_mipsx.go
(1.09 KB)
๐
os_linux_noauxv.go
(408 B)
๐
os_linux_novdso.go
(387 B)
๐
os_linux_ppc64x.go
(566 B)
๐
os_linux_riscv64.go
(198 B)
๐
os_linux_s390x.go
(316 B)
๐
os_linux_x86.go
(270 B)
๐
os_netbsd.go
(9.09 KB)
๐
os_netbsd_386.go
(588 B)
๐
os_netbsd_amd64.go
(585 B)
๐
os_netbsd_arm.go
(1.13 KB)
๐
os_netbsd_arm64.go
(827 B)
๐
os_nonopenbsd.go
(456 B)
๐
os_only_solaris.go
(376 B)
๐
os_openbsd.go
(6.01 KB)
๐
os_openbsd_arm.go
(749 B)
๐
os_openbsd_arm64.go
(416 B)
๐
os_openbsd_libc.go
(1.7 KB)
๐
os_openbsd_mips64.go
(416 B)
๐
os_openbsd_syscall.go
(1.27 KB)
๐
os_openbsd_syscall1.go
(466 B)
๐
os_openbsd_syscall2.go
(2.5 KB)
๐
os_plan9.go
(10.2 KB)
๐
os_plan9_arm.go
(462 B)
๐
os_solaris.go
(6.49 KB)
๐
os_windows.go
(43.68 KB)
๐
os_windows_arm.go
(511 B)
๐
os_windows_arm64.go
(339 B)
๐
panic.go
(44.28 KB)
๐
panic32.go
(4.83 KB)
๐
panic_test.go
(1.71 KB)
๐
plugin.go
(4.27 KB)
๐
pprof
๐
preempt.go
(15.4 KB)
๐
preempt_386.s
(1.07 KB)
๐
preempt_amd64.s
(1.81 KB)
๐
preempt_arm.s
(1.66 KB)
๐
preempt_arm64.s
(2.99 KB)
๐
preempt_mips64x.s
(2.93 KB)
๐
preempt_mipsx.s
(2.89 KB)
๐
preempt_nonwindows.go
(309 B)
๐
preempt_ppc64x.s
(2.92 KB)
๐
preempt_riscv64.s
(2.48 KB)
๐
preempt_s390x.s
(1.19 KB)
๐
preempt_wasm.s
(365 B)
๐
print.go
(5.95 KB)
๐
proc.go
(181.46 KB)
๐
proc_runtime_test.go
(820 B)
๐
proc_test.go
(25.02 KB)
๐
profbuf.go
(18.26 KB)
๐
profbuf_test.go
(8.65 KB)
๐
proflabel.go
(1.52 KB)
๐
race
๐
race.go
(18.56 KB)
๐
race0.go
(2.81 KB)
๐
race_amd64.s
(14.46 KB)
๐
race_arm64.s
(13.71 KB)
๐
race_ppc64le.s
(17.72 KB)
๐
rand_test.go
(783 B)
๐
rdebug.go
(553 B)
๐
relax_stub.go
(617 B)
๐
rt0_aix_ppc64.s
(4.33 KB)
๐
rt0_android_386.s
(822 B)
๐
rt0_android_amd64.s
(754 B)
๐
rt0_android_arm.s
(843 B)
๐
rt0_android_arm64.s
(941 B)
๐
rt0_darwin_amd64.s
(399 B)
๐
rt0_darwin_arm64.s
(2.27 KB)
๐
rt0_dragonfly_amd64.s
(448 B)
๐
rt0_freebsd_386.s
(454 B)
๐
rt0_freebsd_amd64.s
(442 B)
๐
rt0_freebsd_arm.s
(298 B)
๐
rt0_freebsd_arm64.s
(2.46 KB)
๐
rt0_illumos_amd64.s
(311 B)
๐
rt0_ios_amd64.s
(425 B)
๐
rt0_ios_arm64.s
(425 B)
๐
rt0_js_wasm.s
(2.3 KB)
๐
rt0_linux_386.s
(450 B)
๐
rt0_linux_amd64.s
(307 B)
๐
rt0_linux_arm.s
(1007 B)
๐
rt0_linux_arm64.s
(2.39 KB)
๐
rt0_linux_mips64x.s
(1.03 KB)
๐
rt0_linux_mipsx.s
(835 B)
๐
rt0_linux_ppc64.s
(865 B)
๐
rt0_linux_ppc64le.s
(3.88 KB)
๐
rt0_linux_riscv64.s
(370 B)
๐
rt0_linux_s390x.s
(676 B)
๐
rt0_netbsd_386.s
(452 B)
๐
rt0_netbsd_amd64.s
(309 B)
๐
rt0_netbsd_arm.s
(296 B)
๐
rt0_netbsd_arm64.s
(2.38 KB)
๐
rt0_openbsd_386.s
(454 B)
๐
rt0_openbsd_amd64.s
(311 B)
๐
rt0_openbsd_arm.s
(298 B)
๐
rt0_openbsd_arm64.s
(2.54 KB)
๐
rt0_openbsd_mips64.s
(976 B)
๐
rt0_plan9_386.s
(523 B)
๐
rt0_plan9_amd64.s
(481 B)
๐
rt0_plan9_arm.s
(397 B)
๐
rt0_solaris_amd64.s
(311 B)
๐
rt0_windows_386.s
(1.28 KB)
๐
rt0_windows_amd64.s
(986 B)
๐
rt0_windows_arm.s
(386 B)
๐
rt0_windows_arm64.s
(725 B)
๐
runtime-gdb.py
(15.02 KB)
๐
runtime-gdb_test.go
(20.19 KB)
๐
runtime-lldb_test.go
(4.95 KB)
๐
runtime.go
(1.42 KB)
๐
runtime1.go
(12.63 KB)
๐
runtime2.go
(42.27 KB)
๐
runtime_linux_test.go
(1.46 KB)
๐
runtime_mmap_test.go
(1.91 KB)
๐
runtime_test.go
(7.81 KB)
๐
runtime_unix_test.go
(1.29 KB)
๐
rwmutex.go
(3.53 KB)
๐
rwmutex_test.go
(4.03 KB)
๐
select.go
(14.45 KB)
๐
sema.go
(16.08 KB)
๐
sema_test.go
(2.5 KB)
๐
semasleep_test.go
(1.65 KB)
๐
sigaction.go
(543 B)
๐
signal_386.go
(1.72 KB)
๐
signal_aix_ppc64.go
(3.56 KB)
๐
signal_amd64.go
(2.71 KB)
๐
signal_arm.go
(2.56 KB)
๐
signal_arm64.go
(3.16 KB)
๐
signal_darwin.go
(2.13 KB)
๐
signal_darwin_amd64.go
(3.85 KB)
๐
signal_darwin_arm64.go
(3.6 KB)
๐
signal_dragonfly.go
(2.17 KB)
๐
signal_dragonfly_amd64.go
(2.01 KB)
๐
signal_freebsd.go
(2.2 KB)
๐
signal_freebsd_386.go
(1.55 KB)
๐
signal_freebsd_amd64.go
(2.03 KB)
๐
signal_freebsd_arm.go
(2.18 KB)
๐
signal_freebsd_arm64.go
(3.23 KB)
๐
signal_linux_386.go
(1.59 KB)
๐
signal_linux_amd64.go
(2.05 KB)
๐
signal_linux_arm.go
(2.13 KB)
๐
signal_linux_arm64.go
(2.95 KB)
๐
signal_linux_mips64x.go
(3.39 KB)
๐
signal_linux_mipsx.go
(3.7 KB)
๐
signal_linux_ppc64x.go
(3.46 KB)
๐
signal_linux_riscv64.go
(2.92 KB)
๐
signal_linux_s390x.go
(4.43 KB)
๐
signal_mips64x.go
(3.2 KB)
๐
signal_mipsx.go
(3.07 KB)
๐
signal_netbsd.go
(2.18 KB)
๐
signal_netbsd_386.go
(1.76 KB)
๐
signal_netbsd_amd64.go
(2.33 KB)
๐
signal_netbsd_arm.go
(2.3 KB)
๐
signal_netbsd_arm64.go
(3.4 KB)
๐
signal_openbsd.go
(2.18 KB)
๐
signal_openbsd_386.go
(1.58 KB)
๐
signal_openbsd_amd64.go
(2.04 KB)
๐
signal_openbsd_arm.go
(2.12 KB)
๐
signal_openbsd_arm64.go
(3.38 KB)
๐
signal_openbsd_mips64.go
(3.28 KB)
๐
signal_plan9.go
(1.93 KB)
๐
signal_ppc64x.go
(3.64 KB)
๐
signal_riscv64.go
(2.88 KB)
๐
signal_solaris.go
(4.5 KB)
๐
signal_solaris_amd64.go
(2.47 KB)
๐
signal_unix.go
(37.82 KB)
๐
signal_windows.go
(9.2 KB)
๐
signal_windows_test.go
(5.73 KB)
๐
sigqueue.go
(8.76 KB)
๐
sigqueue_note.go
(673 B)
๐
sigqueue_plan9.go
(3.39 KB)
๐
sigtab_aix.go
(11.3 KB)
๐
sigtab_linux_generic.go
(3.56 KB)
๐
sigtab_linux_mipsx.go
(6.01 KB)
๐
sizeclasses.go
(9.14 KB)
๐
sizeof_test.go
(905 B)
๐
slice.go
(8.94 KB)
๐
slice_test.go
(10.32 KB)
๐
softfloat64.go
(10.78 KB)
๐
softfloat64_test.go
(4.05 KB)
๐
stack.go
(41.92 KB)
๐
stack_test.go
(21.05 KB)
๐
string.go
(10.85 KB)
๐
string_test.go
(9.62 KB)
๐
stubs.go
(18.17 KB)
๐
stubs2.go
(1.14 KB)
๐
stubs3.go
(331 B)
๐
stubs_386.go
(550 B)
๐
stubs_amd64.go
(1.2 KB)
๐
stubs_arm.go
(531 B)
๐
stubs_arm64.go
(351 B)
๐
stubs_linux.go
(663 B)
๐
stubs_mips64x.go
(390 B)
๐
stubs_mipsx.go
(305 B)
๐
stubs_nonlinux.go
(315 B)
๐
stubs_ppc64.go
(383 B)
๐
stubs_ppc64le.go
(271 B)
๐
stubs_s390x.go
(256 B)
๐
symtab.go
(32.29 KB)
๐
symtab_test.go
(6.78 KB)
๐
sys_aix_ppc64.s
(7.13 KB)
๐
sys_arm.go
(521 B)
๐
sys_arm64.go
(469 B)
๐
sys_darwin.go
(15.91 KB)
๐
sys_darwin_amd64.s
(18.52 KB)
๐
sys_darwin_arm64.go
(1.68 KB)
๐
sys_darwin_arm64.s
(17.23 KB)
๐
sys_dragonfly_amd64.s
(8.42 KB)
๐
sys_freebsd_386.s
(8.98 KB)
๐
sys_freebsd_amd64.s
(10.55 KB)
๐
sys_freebsd_arm.s
(10.69 KB)
๐
sys_freebsd_arm64.s
(10.33 KB)
๐
sys_libc.go
(1.87 KB)
๐
sys_linux_386.s
(18.17 KB)
๐
sys_linux_amd64.s
(16.25 KB)
๐
sys_linux_arm.s
(15.84 KB)
๐
sys_linux_arm64.s
(15.26 KB)
๐
sys_linux_mips64x.s
(13.4 KB)
๐
sys_linux_mipsx.s
(11.16 KB)
๐
sys_linux_ppc64x.s
(21.48 KB)
๐
sys_linux_riscv64.s
(10.35 KB)
๐
sys_linux_s390x.s
(10.52 KB)
๐
sys_mips64x.go
(526 B)
๐
sys_mipsx.go
(518 B)
๐
sys_netbsd_386.s
(10.13 KB)
๐
sys_netbsd_amd64.s
(9.91 KB)
๐
sys_netbsd_arm.s
(10.94 KB)
๐
sys_netbsd_arm64.s
(10.42 KB)
๐
sys_nonppc64x.go
(271 B)
๐
sys_openbsd.go
(2.3 KB)
๐
sys_openbsd1.go
(1.16 KB)
๐
sys_openbsd2.go
(7.31 KB)
๐
sys_openbsd3.go
(3.29 KB)
๐
sys_openbsd_386.s
(19.97 KB)
๐
sys_openbsd_amd64.s
(16.44 KB)
๐
sys_openbsd_arm.s
(18.09 KB)
๐
sys_openbsd_arm64.s
(15.92 KB)
๐
sys_openbsd_mips64.s
(9.22 KB)
๐
sys_plan9_386.s
(4.4 KB)
๐
sys_plan9_amd64.s
(4.47 KB)
๐
sys_plan9_arm.s
(7.03 KB)
๐
sys_ppc64x.go
(556 B)
๐
sys_riscv64.go
(469 B)
๐
sys_s390x.go
(469 B)
๐
sys_solaris_amd64.s
(6.69 KB)
๐
sys_wasm.go
(732 B)
๐
sys_wasm.s
(2.65 KB)
๐
sys_windows_386.s
(7.74 KB)
๐
sys_windows_amd64.s
(9.16 KB)
๐
sys_windows_arm.s
(12.02 KB)
๐
sys_windows_arm64.s
(12.51 KB)
๐
sys_x86.go
(574 B)
๐
syscall2_solaris.go
(1.65 KB)
๐
syscall_aix.go
(5.99 KB)
๐
syscall_solaris.go
(8.26 KB)
๐
syscall_windows.go
(16.48 KB)
๐
syscall_windows_test.go
(32.53 KB)
๐
testdata
๐
textflag.h
(1.52 KB)
๐
time.go
(30.56 KB)
๐
time_fake.go
(2.38 KB)
๐
time_linux_amd64.s
(2.18 KB)
๐
time_nofake.go
(587 B)
๐
time_test.go
(2.03 KB)
๐
time_windows.h
(694 B)
๐
time_windows_386.s
(1.81 KB)
๐
time_windows_amd64.s
(1.07 KB)
๐
time_windows_arm.s
(2.07 KB)
๐
time_windows_arm64.s
(1.33 KB)
๐
timeasm.go
(468 B)
๐
timestub.go
(595 B)
๐
timestub2.go
(447 B)
๐
tls_arm.s
(3.33 KB)
๐
tls_arm64.h
(1.22 KB)
๐
tls_arm64.s
(1.2 KB)
๐
tls_mips64x.s
(759 B)
๐
tls_mipsx.s
(731 B)
๐
tls_ppc64x.s
(1.52 KB)
๐
tls_riscv64.s
(726 B)
๐
tls_s390x.s
(1.55 KB)
๐
tls_stub.go
(294 B)
๐
tls_windows_amd64.go
(294 B)
๐
trace
๐
trace.go
(38.36 KB)
๐
traceback.go
(46.51 KB)
๐
traceback_test.go
(8.04 KB)
๐
type.go
(18.59 KB)
๐
typekind.go
(742 B)
๐
utf8.go
(3.39 KB)
๐
vdso_elf32.go
(2.79 KB)
๐
vdso_elf64.go
(2.87 KB)
๐
vdso_freebsd.go
(2.46 KB)
๐
vdso_freebsd_arm.go
(454 B)
๐
vdso_freebsd_arm64.go
(443 B)
๐
vdso_freebsd_x86.go
(1.89 KB)
๐
vdso_in_none.go
(490 B)
๐
vdso_linux.go
(7.77 KB)
๐
vdso_linux_386.go
(669 B)
๐
vdso_linux_amd64.go
(685 B)
๐
vdso_linux_arm.go
(669 B)
๐
vdso_linux_arm64.go
(670 B)
๐
vdso_linux_mips64x.go
(892 B)
๐
vdso_linux_ppc64x.go
(712 B)
๐
vlop_386.s
(2.02 KB)
๐
vlop_arm.s
(7.06 KB)
๐
vlop_arm_test.go
(3.75 KB)
๐
vlrt.go
(5.91 KB)
๐
wincallback.go
(3.52 KB)
๐
write_err.go
(310 B)
๐
write_err_android.go
(4.65 KB)
๐
zcallback_windows.go
(155 B)
๐
zcallback_windows.s
(63.05 KB)
๐
zcallback_windows_arm.s
(89.34 KB)
๐
zcallback_windows_arm64.s
(89.34 KB)
Editing: race_amd64.s
// Copyright 2013 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. //go:build race // +build race #include "go_asm.h" #include "go_tls.h" #include "funcdata.h" #include "textflag.h" #include "cgo/abi_amd64.h" // The following thunks allow calling the gcc-compiled race runtime directly // from Go code without going all the way through cgo. // First, it's much faster (up to 50% speedup for real Go programs). // Second, it eliminates race-related special cases from cgocall and scheduler. // Third, in long-term it will allow to remove cyclic runtime/race dependency on cmd/go. // A brief recap of the amd64 calling convention. // Arguments are passed in DI, SI, DX, CX, R8, R9, the rest is on stack. // Callee-saved registers are: BX, BP, R12-R15. // SP must be 16-byte aligned. // On Windows: // Arguments are passed in CX, DX, R8, R9, the rest is on stack. // Callee-saved registers are: BX, BP, DI, SI, R12-R15. // SP must be 16-byte aligned. Windows also requires "stack-backing" for the 4 register arguments: // https://msdn.microsoft.com/en-us/library/ms235286.aspx // We do not do this, because it seems to be intended for vararg/unprototyped functions. // Gcc-compiled race runtime does not try to use that space. #ifdef GOOS_windows #define RARG0 CX #define RARG1 DX #define RARG2 R8 #define RARG3 R9 #else #define RARG0 DI #define RARG1 SI #define RARG2 DX #define RARG3 CX #endif // func runtimeยทraceread(addr uintptr) // Called from instrumented code. // Defined as ABIInternal so as to avoid introducing a wrapper, // which would render runtime.getcallerpc ineffective. TEXT runtimeยทraceread<ABIInternal>(SB), NOSPLIT, $0-8 #ifdef GOEXPERIMENT_regabiargs MOVQ AX, RARG1 #else MOVQ addr+0(FP), RARG1 #endif MOVQ (SP), RARG2 // void __tsan_read(ThreadState *thr, void *addr, void *pc); MOVQ $__tsan_read(SB), AX JMP racecalladdr<>(SB) // func runtimeยทRaceRead(addr uintptr) TEXT runtimeยทRaceRead(SB), NOSPLIT, $0-8 // This needs to be a tail call, because raceread reads caller pc. JMP runtimeยทraceread(SB) // void runtimeยทracereadpc(void *addr, void *callpc, void *pc) TEXT runtimeยทracereadpc(SB), NOSPLIT, $0-24 MOVQ addr+0(FP), RARG1 MOVQ callpc+8(FP), RARG2 MOVQ pc+16(FP), RARG3 ADDQ $1, RARG3 // pc is function start, tsan wants return address // void __tsan_read_pc(ThreadState *thr, void *addr, void *callpc, void *pc); MOVQ $__tsan_read_pc(SB), AX JMP racecalladdr<>(SB) // func runtimeยทracewrite(addr uintptr) // Called from instrumented code. // Defined as ABIInternal so as to avoid introducing a wrapper, // which would render runtime.getcallerpc ineffective. TEXT runtimeยทracewrite<ABIInternal>(SB), NOSPLIT, $0-8 #ifdef GOEXPERIMENT_regabiargs MOVQ AX, RARG1 #else MOVQ addr+0(FP), RARG1 #endif MOVQ (SP), RARG2 // void __tsan_write(ThreadState *thr, void *addr, void *pc); MOVQ $__tsan_write(SB), AX JMP racecalladdr<>(SB) // func runtimeยทRaceWrite(addr uintptr) TEXT runtimeยทRaceWrite(SB), NOSPLIT, $0-8 // This needs to be a tail call, because racewrite reads caller pc. JMP runtimeยทracewrite(SB) // void runtimeยทracewritepc(void *addr, void *callpc, void *pc) TEXT runtimeยทracewritepc(SB), NOSPLIT, $0-24 MOVQ addr+0(FP), RARG1 MOVQ callpc+8(FP), RARG2 MOVQ pc+16(FP), RARG3 ADDQ $1, RARG3 // pc is function start, tsan wants return address // void __tsan_write_pc(ThreadState *thr, void *addr, void *callpc, void *pc); MOVQ $__tsan_write_pc(SB), AX JMP racecalladdr<>(SB) // func runtimeยทracereadrange(addr, size uintptr) // Called from instrumented code. TEXT runtimeยทracereadrange(SB), NOSPLIT, $0-16 MOVQ addr+0(FP), RARG1 MOVQ size+8(FP), RARG2 MOVQ (SP), RARG3 // void __tsan_read_range(ThreadState *thr, void *addr, uintptr size, void *pc); MOVQ $__tsan_read_range(SB), AX JMP racecalladdr<>(SB) // func runtimeยทRaceReadRange(addr, size uintptr) TEXT runtimeยทRaceReadRange(SB), NOSPLIT, $0-16 // This needs to be a tail call, because racereadrange reads caller pc. JMP runtimeยทracereadrange(SB) // void runtimeยทracereadrangepc1(void *addr, uintptr sz, void *pc) TEXT runtimeยทracereadrangepc1(SB), NOSPLIT, $0-24 MOVQ addr+0(FP), RARG1 MOVQ size+8(FP), RARG2 MOVQ pc+16(FP), RARG3 ADDQ $1, RARG3 // pc is function start, tsan wants return address // void __tsan_read_range(ThreadState *thr, void *addr, uintptr size, void *pc); MOVQ $__tsan_read_range(SB), AX JMP racecalladdr<>(SB) // func runtimeยทracewriterange(addr, size uintptr) // Called from instrumented code. // Defined as ABIInternal so as to avoid introducing a wrapper, // which would render runtime.getcallerpc ineffective. TEXT runtimeยทracewriterange<ABIInternal>(SB), NOSPLIT, $0-16 #ifdef GOEXPERIMENT_regabiargs MOVQ AX, RARG1 MOVQ BX, RARG2 #else MOVQ addr+0(FP), RARG1 MOVQ size+8(FP), RARG2 #endif MOVQ (SP), RARG3 // void __tsan_write_range(ThreadState *thr, void *addr, uintptr size, void *pc); MOVQ $__tsan_write_range(SB), AX JMP racecalladdr<>(SB) // func runtimeยทRaceWriteRange(addr, size uintptr) TEXT runtimeยทRaceWriteRange(SB), NOSPLIT, $0-16 // This needs to be a tail call, because racewriterange reads caller pc. JMP runtimeยทracewriterange(SB) // void runtimeยทracewriterangepc1(void *addr, uintptr sz, void *pc) TEXT runtimeยทracewriterangepc1(SB), NOSPLIT, $0-24 MOVQ addr+0(FP), RARG1 MOVQ size+8(FP), RARG2 MOVQ pc+16(FP), RARG3 ADDQ $1, RARG3 // pc is function start, tsan wants return address // void __tsan_write_range(ThreadState *thr, void *addr, uintptr size, void *pc); MOVQ $__tsan_write_range(SB), AX JMP racecalladdr<>(SB) // If addr (RARG1) is out of range, do nothing. // Otherwise, setup goroutine context and invoke racecall. Other arguments already set. TEXT racecalladdr<>(SB), NOSPLIT, $0-0 #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_racectx(R14), RARG0 // goroutine context // Check that addr is within [arenastart, arenaend) or within [racedatastart, racedataend). CMPQ RARG1, runtimeยทracearenastart(SB) JB data CMPQ RARG1, runtimeยทracearenaend(SB) JB call data: CMPQ RARG1, runtimeยทracedatastart(SB) JB ret CMPQ RARG1, runtimeยทracedataend(SB) JAE ret call: MOVQ AX, AX // w/o this 6a miscompiles this function JMP racecall<>(SB) ret: RET // func runtimeยทracefuncenter(pc uintptr) // Called from instrumented code. TEXT runtimeยทracefuncenter(SB), NOSPLIT, $0-8 MOVQ callpc+0(FP), R11 JMP racefuncenter<>(SB) // Common code for racefuncenter // R11 = caller's return address TEXT racefuncenter<>(SB), NOSPLIT, $0-0 MOVQ DX, BX // save function entry context (for closures) #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_racectx(R14), RARG0 // goroutine context MOVQ R11, RARG1 // void __tsan_func_enter(ThreadState *thr, void *pc); MOVQ $__tsan_func_enter(SB), AX // racecall<> preserves BX CALL racecall<>(SB) MOVQ BX, DX // restore function entry context RET // func runtimeยทracefuncexit() // Called from instrumented code. TEXT runtimeยทracefuncexit(SB), NOSPLIT, $0-0 #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_racectx(R14), RARG0 // goroutine context // void __tsan_func_exit(ThreadState *thr); MOVQ $__tsan_func_exit(SB), AX JMP racecall<>(SB) // Atomic operations for sync/atomic package. // Load TEXT syncโatomicยทLoadInt32(SB), NOSPLIT, $0-12 GO_ARGS MOVQ $__tsan_go_atomic32_load(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทLoadInt64(SB), NOSPLIT, $0-16 GO_ARGS MOVQ $__tsan_go_atomic64_load(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทLoadUint32(SB), NOSPLIT, $0-12 GO_ARGS JMP syncโatomicยทLoadInt32(SB) TEXT syncโatomicยทLoadUint64(SB), NOSPLIT, $0-16 GO_ARGS JMP syncโatomicยทLoadInt64(SB) TEXT syncโatomicยทLoadUintptr(SB), NOSPLIT, $0-16 GO_ARGS JMP syncโatomicยทLoadInt64(SB) TEXT syncโatomicยทLoadPointer(SB), NOSPLIT, $0-16 GO_ARGS JMP syncโatomicยทLoadInt64(SB) // Store TEXT syncโatomicยทStoreInt32(SB), NOSPLIT, $0-12 GO_ARGS MOVQ $__tsan_go_atomic32_store(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทStoreInt64(SB), NOSPLIT, $0-16 GO_ARGS MOVQ $__tsan_go_atomic64_store(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทStoreUint32(SB), NOSPLIT, $0-12 GO_ARGS JMP syncโatomicยทStoreInt32(SB) TEXT syncโatomicยทStoreUint64(SB), NOSPLIT, $0-16 GO_ARGS JMP syncโatomicยทStoreInt64(SB) TEXT syncโatomicยทStoreUintptr(SB), NOSPLIT, $0-16 GO_ARGS JMP syncโatomicยทStoreInt64(SB) // Swap TEXT syncโatomicยทSwapInt32(SB), NOSPLIT, $0-20 GO_ARGS MOVQ $__tsan_go_atomic32_exchange(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทSwapInt64(SB), NOSPLIT, $0-24 GO_ARGS MOVQ $__tsan_go_atomic64_exchange(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทSwapUint32(SB), NOSPLIT, $0-20 GO_ARGS JMP syncโatomicยทSwapInt32(SB) TEXT syncโatomicยทSwapUint64(SB), NOSPLIT, $0-24 GO_ARGS JMP syncโatomicยทSwapInt64(SB) TEXT syncโatomicยทSwapUintptr(SB), NOSPLIT, $0-24 GO_ARGS JMP syncโatomicยทSwapInt64(SB) // Add TEXT syncโatomicยทAddInt32(SB), NOSPLIT, $0-20 GO_ARGS MOVQ $__tsan_go_atomic32_fetch_add(SB), AX CALL racecallatomic<>(SB) MOVL add+8(FP), AX // convert fetch_add to add_fetch ADDL AX, ret+16(FP) RET TEXT syncโatomicยทAddInt64(SB), NOSPLIT, $0-24 GO_ARGS MOVQ $__tsan_go_atomic64_fetch_add(SB), AX CALL racecallatomic<>(SB) MOVQ add+8(FP), AX // convert fetch_add to add_fetch ADDQ AX, ret+16(FP) RET TEXT syncโatomicยทAddUint32(SB), NOSPLIT, $0-20 GO_ARGS JMP syncโatomicยทAddInt32(SB) TEXT syncโatomicยทAddUint64(SB), NOSPLIT, $0-24 GO_ARGS JMP syncโatomicยทAddInt64(SB) TEXT syncโatomicยทAddUintptr(SB), NOSPLIT, $0-24 GO_ARGS JMP syncโatomicยทAddInt64(SB) // CompareAndSwap TEXT syncโatomicยทCompareAndSwapInt32(SB), NOSPLIT, $0-17 GO_ARGS MOVQ $__tsan_go_atomic32_compare_exchange(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทCompareAndSwapInt64(SB), NOSPLIT, $0-25 GO_ARGS MOVQ $__tsan_go_atomic64_compare_exchange(SB), AX CALL racecallatomic<>(SB) RET TEXT syncโatomicยทCompareAndSwapUint32(SB), NOSPLIT, $0-17 GO_ARGS JMP syncโatomicยทCompareAndSwapInt32(SB) TEXT syncโatomicยทCompareAndSwapUint64(SB), NOSPLIT, $0-25 GO_ARGS JMP syncโatomicยทCompareAndSwapInt64(SB) TEXT syncโatomicยทCompareAndSwapUintptr(SB), NOSPLIT, $0-25 GO_ARGS JMP syncโatomicยทCompareAndSwapInt64(SB) // Generic atomic operation implementation. // AX already contains target function. TEXT racecallatomic<>(SB), NOSPLIT, $0-0 // Trigger SIGSEGV early. MOVQ 16(SP), R12 MOVL (R12), R13 // Check that addr is within [arenastart, arenaend) or within [racedatastart, racedataend). CMPQ R12, runtimeยทracearenastart(SB) JB racecallatomic_data CMPQ R12, runtimeยทracearenaend(SB) JB racecallatomic_ok racecallatomic_data: CMPQ R12, runtimeยทracedatastart(SB) JB racecallatomic_ignore CMPQ R12, runtimeยทracedataend(SB) JAE racecallatomic_ignore racecallatomic_ok: // Addr is within the good range, call the atomic function. #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_racectx(R14), RARG0 // goroutine context MOVQ 8(SP), RARG1 // caller pc MOVQ (SP), RARG2 // pc LEAQ 16(SP), RARG3 // arguments JMP racecall<>(SB) // does not return racecallatomic_ignore: // Addr is outside the good range. // Call __tsan_go_ignore_sync_begin to ignore synchronization during the atomic op. // An attempt to synchronize on the address would cause crash. MOVQ AX, BX // remember the original function MOVQ $__tsan_go_ignore_sync_begin(SB), AX #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_racectx(R14), RARG0 // goroutine context CALL racecall<>(SB) MOVQ BX, AX // restore the original function // Call the atomic function. MOVQ g_racectx(R14), RARG0 // goroutine context MOVQ 8(SP), RARG1 // caller pc MOVQ (SP), RARG2 // pc LEAQ 16(SP), RARG3 // arguments CALL racecall<>(SB) // Call __tsan_go_ignore_sync_end. MOVQ $__tsan_go_ignore_sync_end(SB), AX MOVQ g_racectx(R14), RARG0 // goroutine context JMP racecall<>(SB) // void runtimeยทracecall(void(*f)(...), ...) // Calls C function f from race runtime and passes up to 4 arguments to it. // The arguments are never heap-object-preserving pointers, so we pretend there are no arguments. TEXT runtimeยทracecall(SB), NOSPLIT, $0-0 MOVQ fn+0(FP), AX MOVQ arg0+8(FP), RARG0 MOVQ arg1+16(FP), RARG1 MOVQ arg2+24(FP), RARG2 MOVQ arg3+32(FP), RARG3 JMP racecall<>(SB) // Switches SP to g0 stack and calls (AX). Arguments already set. TEXT racecall<>(SB), NOSPLIT, $0-0 #ifndef GOEXPERIMENT_regabig get_tls(R12) MOVQ g(R12), R14 #endif MOVQ g_m(R14), R13 // Switch to g0 stack. MOVQ SP, R12 // callee-saved, preserved across the CALL MOVQ m_g0(R13), R10 CMPQ R10, R14 JE call // already on g0 MOVQ (g_sched+gobuf_sp)(R10), SP call: ANDQ $~15, SP // alignment for gcc ABI CALL AX MOVQ R12, SP // Back to Go world, set special registers. // The g register (R14) is preserved in C. XORPS X15, X15 RET // C->Go callback thunk that allows to call runtimeยทracesymbolize from C code. // Direct Go->C race call has only switched SP, finish g->g0 switch by setting correct g. // The overall effect of Go->C->Go call chain is similar to that of mcall. // RARG0 contains command code. RARG1 contains command-specific context. // See racecallback for command codes. // Defined as ABIInternal so as to avoid introducing a wrapper, // because its address is passed to C via funcPC. TEXT runtimeยทracecallbackthunk<ABIInternal>(SB), NOSPLIT, $0-0 // Handle command raceGetProcCmd (0) here. // First, code below assumes that we are on curg, while raceGetProcCmd // can be executed on g0. Second, it is called frequently, so will // benefit from this fast path. CMPQ RARG0, $0 JNE rest get_tls(RARG0) MOVQ g(RARG0), RARG0 MOVQ g_m(RARG0), RARG0 MOVQ m_p(RARG0), RARG0 MOVQ p_raceprocctx(RARG0), RARG0 MOVQ RARG0, (RARG1) RET rest: // Transition from C ABI to Go ABI. PUSH_REGS_HOST_TO_ABI0() // Set g = g0. get_tls(R12) MOVQ g(R12), R14 MOVQ g_m(R14), R13 MOVQ m_g0(R13), R15 CMPQ R13, R15 JEQ noswitch // branch if already on g0 MOVQ R15, g(R12) // g = m->g0 MOVQ R15, R14 // set g register PUSHQ RARG1 // func arg PUSHQ RARG0 // func arg CALL runtimeยทracecallback(SB) POPQ R12 POPQ R12 // All registers are smashed after Go code, reload. get_tls(R12) MOVQ g(R12), R13 MOVQ g_m(R13), R13 MOVQ m_curg(R13), R14 MOVQ R14, g(R12) // g = m->curg ret: POP_REGS_HOST_TO_ABI0() RET noswitch: // already on g0 PUSHQ RARG1 // func arg PUSHQ RARG0 // func arg CALL runtimeยทracecallback(SB) POPQ R12 POPQ R12 JMP ret
Upload File
Create Folder