1
0
mirror of https://github.com/golang/go synced 2024-11-07 12:26:16 -07:00
go/src/runtime
Austin Clements c19759aa48 runtime: eliminate externalthreadhandler
This function is no longer used.

Eliminating this actually fixes several problems:

- It made assumptions about what registers memclrNoHeapPointers would
  preserve. Besides being an abstraction violation and lurking
  maintenance issue, this actively became a problem for regabi because
  the call to memclrNoHeapPointers now happens through an ABI wrapper,
  which is generated by the compiler and hence we can't easily control
  what registers it clobbers.

- The amd64 implementation (at least), does not interact with the host
  ABI correctly. Notably, it doesn't save many of the registers that
  are callee-save in the host ABI but caller-save in the Go ABI.

- It interacts strangely with the NOSPLIT checker because it allocates
  an entire M and G on its stack. It worked around this on arm64, and
  happened to do things the NOSPLIT checker couldn't track on 386 and
  amd64, and happened to be *4 bytes* below the limit on arm (so any
  addition to the m or g structs would cause a NOSPLIT failure). See
  CL 309031 for a more complete explanation.

Fixes #45530.
Updates #40724.

Change-Id: Ic70d4d7e1c17f1d796575b3377b8529449e93576
Reviewed-on: https://go-review.googlesource.com/c/go/+/309634
Trust: Austin Clements <austin@google.com>
Run-TryBot: Austin Clements <austin@google.com>
TryBot-Result: Go Bot <gobot@golang.org>
Reviewed-by: Michael Pratt <mpratt@google.com>
Reviewed-by: Michael Knyszek <mknyszek@google.com>
2021-04-13 21:13:12 +00:00
..
cgo all: simplify the spelling of Linux 2021-04-13 13:56:21 +00:00
debug all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
internal runtime: using wyhash for memhashFallback on 64bit platform 2021-04-12 02:29:32 +00:00
metrics runtime/metrics: update documentation to current interface 2021-02-16 16:26:30 +00:00
msan
pprof runtime/pprof: deflake TestMorestack 2021-04-06 18:01:39 +00:00
race runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
testdata all: run gofmt 2021-03-15 21:49:19 +00:00
trace
abi_test.go all: explode GOEXPERIMENT=regabi into 5 sub-experiments 2021-03-18 16:51:27 +00:00
alg.go
asm_386.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_amd64.s runtime: port performance-critical functions to regabi 2021-04-12 18:08:47 +00:00
asm_arm64.s cmd/compile: mark R16, R17 clobbered for non-standard calls on ARM64 2021-03-25 21:30:55 +00:00
asm_arm.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_mips64x.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_mipsx.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_ppc64x.h
asm_ppc64x.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_riscv64.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_s390x.s runtime: fix spurious stack overflow detection 2021-02-19 15:30:52 +00:00
asm_wasm.s runtime: use TOPFRAME to identify top-of-frame functions 2021-02-19 00:02:49 +00:00
asm.s [dev.regabi] runtime: initialize special registers before sigpanic 2021-02-08 17:48:48 +00:00
atomic_arm64.s
atomic_mips64x.s
atomic_mipsx.s
atomic_pointer.go
atomic_ppc64x.s
atomic_riscv64.s
auxv_none.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
callers_test.go
cgo_mmap.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
cgo_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
cgo_sigaction.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
cgo.go
cgocall.go runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
cgocallback.go
cgocheck.go
chan_test.go docs: fix spelling 2021-02-24 04:11:43 +00:00
chan.go cmd/compile,runtime: make selectnbrecv return two values 2021-02-23 05:02:26 +00:00
chanbarrier_test.go
checkptr_test.go
checkptr.go
closure_test.go
compiler.go
complex_test.go
complex.go
conv_wasm_test.go
cpuflags_amd64.go
cpuflags_arm64.go
cpuflags.go
cpuprof.go runtime: handle nil gp in cpuprof 2021-02-19 00:01:52 +00:00
cputicks.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
crash_cgo_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
crash_nonunix_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
crash_test.go runtime: make sure to remove open-coded defer entries in all cases after a recover 2021-01-27 20:44:24 +00:00
crash_unix_test.go runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
debug_test.go runtime: move zero-sized frame check from newproc to newproc1 2021-04-11 20:07:18 +00:00
debug.go
debugcall.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
debuglog_off.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
debuglog_on.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
debuglog_test.go
debuglog.go
defer_test.go all: remove duplicate words 2021-03-13 11:56:59 +00:00
defs1_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs1_netbsd_386.go
defs1_netbsd_amd64.go
defs1_netbsd_arm64.go
defs1_netbsd_arm.go
defs1_solaris_amd64.go
defs2_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs3_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_aix_ppc64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_aix.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_arm_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_darwin_amd64.go
defs_darwin_arm64.go
defs_darwin.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_dragonfly_amd64.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
defs_dragonfly.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
defs_freebsd_386.go
defs_freebsd_amd64.go
defs_freebsd_arm64.go
defs_freebsd_arm.go
defs_freebsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_illumos_amd64.go
defs_linux_386.go
defs_linux_amd64.go
defs_linux_arm64.go
defs_linux_arm.go
defs_linux_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_linux_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_linux_ppc64.go
defs_linux_ppc64le.go
defs_linux_riscv64.go
defs_linux_s390x.go
defs_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_netbsd_386.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_netbsd_amd64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_netbsd_arm.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_netbsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_openbsd_386.go
defs_openbsd_amd64.go runtime: switch runtime to libc for openbsd/amd64 2021-01-22 18:58:08 +00:00
defs_openbsd_arm64.go runtime: switch runtime to libc for openbsd/arm64 2021-01-27 12:18:00 +00:00
defs_openbsd_arm.go
defs_openbsd_mips64.go
defs_openbsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_plan9_386.go
defs_plan9_amd64.go
defs_plan9_arm.go
defs_solaris_amd64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_solaris.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
defs_windows_386.go runtime: factor common code out of defs_windows_*.go 2021-02-19 00:03:30 +00:00
defs_windows_amd64.go runtime: factor common code out of defs_windows_*.go 2021-02-19 00:03:30 +00:00
defs_windows_arm64.go runtime: initial windows/arm64 implementation files 2021-02-19 00:40:56 +00:00
defs_windows_arm.go runtime: fix windows/arm CONTEXT_CONTROL 2021-02-19 00:03:36 +00:00
defs_windows.go runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
duff_386.s
duff_amd64.s [dev.regabi] cmd/compile: reserve X15 as zero register on AMD64 2021-02-03 22:44:53 +00:00
duff_arm64.s
duff_arm.s
duff_mips64x.s
duff_ppc64x.s
duff_riscv64.s
duff_s390x.s
env_plan9.go
env_posix.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
env_test.go
error.go
example_test.go
export_aix_test.go
export_arm_test.go
export_darwin_test.go
export_debug_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
export_debuglog_test.go
export_futex_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
export_linux_test.go
export_mmap_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
export_pipe2_test.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
export_pipe_test.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
export_solaris_test.go
export_test.go runtime: support register ABI Go functions from Windows callbacks 2021-03-31 20:09:03 +00:00
export_unix_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
export_windows_test.go
extern.go runtime,cmd/link: include GOEXPERIMENTs in runtime.Version(), "go version X" 2021-04-08 02:17:22 +00:00
fastlog2_test.go
fastlog2.go
fastlog2table.go
float.go
funcdata.h
futex_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
gc_test.go runtime: make gcTestMoveStackOnNextCall not double the stack 2021-04-02 01:14:00 +00:00
gcinfo_test.go
go_tls.h
HACKING.md
hash32.go runtime: using wyhash for memhashFallback on 32bit platform 2021-03-16 00:50:54 +00:00
hash64.go runtime: using wyhash for memhashFallback on 64bit platform 2021-04-12 02:29:32 +00:00
hash_test.go
heapdump.go runtime: drop haveexperiment, sys.GOEXPERIMENT 2021-04-08 02:17:13 +00:00
histogram_test.go
histogram.go runtime: fix typo in histogram.go 2021-02-04 04:46:49 +00:00
iface_test.go
iface.go cmd/compile: make interface conversion function selection ABI insensitive 2021-04-12 22:50:31 +00:00
lfstack_32bit.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lfstack_64bit.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lfstack_test.go
lfstack.go
libfuzzer_amd64.s
libfuzzer_arm64.s
libfuzzer.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lock_futex.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lock_js.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lock_sema.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lockrank_off.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
lockrank_on.go runtime: check partial lock ranking order 2021-03-10 19:07:29 +00:00
lockrank_test.go runtime: check partial lock ranking order 2021-03-10 19:07:29 +00:00
lockrank.go runtime: check partial lock ranking order 2021-03-10 19:07:29 +00:00
Makefile
malloc_test.go
malloc.go runtime: fix typos in comments 2021-03-30 03:31:44 +00:00
map_benchmark_test.go
map_fast32.go
map_fast64.go
map_faststr.go runtime: overwrite existing keys for mapassign_faststr variant 2021-03-28 03:27:04 +00:00
map_test.go
map.go runtime: simplify syntax for pointer arithmetic in mapaccess functions 2021-04-11 20:41:32 +00:00
mbarrier.go [dev.regabi] reflect: support for register ABI on amd64 for reflect.(Value).Call 2021-02-16 15:51:50 +00:00
mbitmap.go runtime: simplify divmagic for span calculations 2021-03-12 18:02:59 +00:00
mcache.go
mcentral.go runtime: block sweep completion on all sweep paths 2021-04-12 19:22:50 +00:00
mcheckmark.go
mem_aix.go
mem_bsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mem_darwin.go
mem_js.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mem_linux.go
mem_plan9.go
mem_windows.go
memclr_386.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
memclr_amd64.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
memclr_arm64.s runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
memclr_arm.s runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
memclr_mips64x.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_mipsx.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_plan9_386.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_plan9_amd64.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_ppc64x.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_riscv64.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_s390x.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memclr_wasm.s runtime: document pointer write atomicity for memclrNoHeapPointers 2021-01-29 19:11:07 +00:00
memmove_386.s
memmove_amd64.s runtime: port performance-critical functions to regabi 2021-04-12 18:08:47 +00:00
memmove_arm64.s
memmove_arm.s
memmove_linux_amd64_test.go
memmove_mips64x.s
memmove_mipsx.s
memmove_plan9_386.s
memmove_plan9_amd64.s
memmove_ppc64x.s all: remove duplicate words 2021-03-13 11:56:59 +00:00
memmove_riscv64.s
memmove_s390x.s
memmove_test.go
memmove_wasm.s
metrics_test.go
metrics.go docs: fix spelling 2021-02-24 04:11:43 +00:00
mfinal_test.go
mfinal.go runtime: support register ABI for finalizers 2021-03-11 17:26:22 +00:00
mfixalloc.go
mgc.go runtime: consolidate "is sweep done" conditions 2021-04-12 19:22:52 +00:00
mgcmark.go runtime: encapsulate access to allgs 2021-03-05 22:09:52 +00:00
mgcscavenge_test.go runtime: remove a duplicated testcase of TestPallocDataFindScavengeCa… 2021-03-04 16:31:19 +00:00
mgcscavenge.go cmd/compile: wrap/desugar defer calls for register abi 2021-03-23 23:08:19 +00:00
mgcstack.go
mgcsweep.go runtime: consolidate "is sweep done" conditions 2021-04-12 19:22:52 +00:00
mgcwork.go runtime: fix some typos 2021-03-29 19:16:20 +00:00
mheap.go runtime: consolidate "is sweep done" conditions 2021-04-12 19:22:52 +00:00
mkduff.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mkfastlog2table.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mkpreempt.go runtime: save R15 before checking AVX state 2021-02-23 20:05:37 +00:00
mksizeclasses.go runtime: fix documented alignment of 32KiB and 64KiB size classes 2021-03-13 04:53:32 +00:00
mmap.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mpagealloc_32bit.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mpagealloc_64bit.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
mpagealloc_test.go
mpagealloc.go runtime: check for sysAlloc failures in pageAlloc 2021-03-31 03:52:40 +00:00
mpagecache_test.go
mpagecache.go
mpallocbits_test.go
mpallocbits.go
mprof.go runtime, cmd/link/internal/ld: disable memory profiling when data unreachable 2021-03-09 20:09:52 +00:00
mranges_test.go
mranges.go
msan0.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
msan_amd64.s
msan_arm64.s
msan.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
msize.go
mspanset.go
mstats.go
mwbbuf.go
nbpipe_fcntl_libc_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
nbpipe_fcntl_unix_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
nbpipe_pipe2.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
nbpipe_pipe.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
nbpipe_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
net_plan9.go
netpoll_aix.go
netpoll_epoll.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
netpoll_fake.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
netpoll_kqueue.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
netpoll_os_test.go
netpoll_solaris.go
netpoll_stub.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
netpoll_windows.go
netpoll.go runtime: document netpollclose 2021-03-09 07:44:18 +00:00
norace_linux_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
norace_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
numcpu_freebsd_test.go
os2_aix.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
os2_freebsd.go
os2_openbsd.go
os2_plan9.go
os2_solaris.go
os3_plan9.go runtime: use sigpanic0 on all OSes 2021-04-09 17:49:01 +00:00
os3_solaris.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
os_aix.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_android.go
os_darwin_arm64.go
os_darwin.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
os_dragonfly.go runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
os_freebsd2.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_freebsd_amd64.go
os_freebsd_arm64.go
os_freebsd_arm.go
os_freebsd_noauxv.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_freebsd.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
os_illumos.go
os_js.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_arm64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_arm.go
os_linux_be64.go all: simplify the spelling of Linux 2021-04-13 13:56:21 +00:00
os_linux_generic.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_noauxv.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_novdso.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux_riscv64.go
os_linux_s390x.go
os_linux_x86.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_linux.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
os_netbsd_386.go
os_netbsd_amd64.go
os_netbsd_arm64.go
os_netbsd_arm.go
os_netbsd.go runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
os_nonopenbsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_only_solaris.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_openbsd_arm64.go
os_openbsd_arm.go
os_openbsd_libc.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_openbsd_mips64.go
os_openbsd_syscall1.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_openbsd_syscall2.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_openbsd_syscall.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
os_openbsd.go runtime: switch runtime to libc for openbsd/amd64 2021-01-22 18:58:08 +00:00
os_plan9_arm.go
os_plan9.go runtime: init plan9 hashkey by time 2021-03-30 01:17:14 +00:00
os_solaris.go
os_windows_arm64.go runtime: initial windows/arm64 implementation files 2021-02-19 00:40:56 +00:00
os_windows_arm.go
os_windows.go runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
panic32.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
panic_test.go
panic.go runtime: remove deferreturn dummy argument 2021-04-12 16:30:17 +00:00
plugin.go
preempt_386.s
preempt_amd64.s runtime: save R15 before checking AVX state 2021-02-23 20:05:37 +00:00
preempt_arm64.s
preempt_arm.s
preempt_mips64x.s
preempt_mipsx.s
preempt_nonwindows.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
preempt_ppc64x.s
preempt_riscv64.s
preempt_s390x.s
preempt_wasm.s
preempt.go
print.go runtime: print hex numbers with hex prefixes in traceback debug 2021-02-19 00:03:44 +00:00
proc_runtime_test.go
proc_test.go
proc.go runtime: move zero-sized frame check from newproc to newproc1 2021-04-11 20:07:18 +00:00
profbuf_test.go
profbuf.go
proflabel.go
race0.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
race_amd64.s cmd/asm,runtime: reduce spellings of GOEXPERIMENTs 2021-04-08 02:17:15 +00:00
race_arm64.s runtime: remove racefuncenterfp 2021-03-05 23:32:44 +00:00
race_ppc64le.s cmd/link: support 32b TLS_LE offsets on PPC64 2021-04-13 13:54:51 +00:00
race.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
rand_test.go
rdebug.go
relax_stub.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
rt0_aix_ppc64.s
rt0_android_386.s
rt0_android_amd64.s
rt0_android_arm64.s
rt0_android_arm.s
rt0_darwin_amd64.s
rt0_darwin_arm64.s
rt0_dragonfly_amd64.s
rt0_freebsd_386.s
rt0_freebsd_amd64.s
rt0_freebsd_arm64.s
rt0_freebsd_arm.s
rt0_illumos_amd64.s
rt0_ios_amd64.s
rt0_ios_arm64.s
rt0_js_wasm.s
rt0_linux_386.s
rt0_linux_amd64.s
rt0_linux_arm64.s
rt0_linux_arm.s
rt0_linux_mips64x.s
rt0_linux_mipsx.s
rt0_linux_ppc64.s
rt0_linux_ppc64le.s
rt0_linux_riscv64.s
rt0_linux_s390x.s
rt0_netbsd_386.s
rt0_netbsd_amd64.s
rt0_netbsd_arm64.s
rt0_netbsd_arm.s
rt0_openbsd_386.s
rt0_openbsd_amd64.s
rt0_openbsd_arm64.s
rt0_openbsd_arm.s
rt0_openbsd_mips64.s
rt0_plan9_386.s
rt0_plan9_amd64.s
rt0_plan9_arm.s
rt0_solaris_amd64.s
rt0_windows_386.s
rt0_windows_amd64.s runtime: fix stack alignment for Windows amd64 lib entry 2021-03-20 17:08:03 +00:00
rt0_windows_arm64.s runtime: initial windows/arm64 implementation files 2021-02-19 00:40:56 +00:00
rt0_windows_arm.s
runtime1.go runtime: remove GODEBUG=scavenge mode 2021-03-04 17:27:32 +00:00
runtime2.go runtime: set up read-only dummy TLS space for needm on Windows 2021-04-08 16:37:24 +00:00
runtime_linux_test.go
runtime_mmap_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
runtime_test.go runtime: document, clean up internal/sys 2021-02-19 00:01:38 +00:00
runtime_unix_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
runtime-gdb_test.go runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
runtime-gdb.py
runtime-lldb_test.go runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
runtime.go
rwmutex_test.go
rwmutex.go
select.go
sema_test.go
sema.go
semasleep_test.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sigaction.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_386.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_aix_ppc64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_amd64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_arm64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_arm.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_darwin_amd64.go
signal_darwin_arm64.go
signal_darwin.go
signal_dragonfly_amd64.go
signal_dragonfly.go
signal_freebsd_386.go
signal_freebsd_amd64.go
signal_freebsd_arm64.go
signal_freebsd_arm.go
signal_freebsd.go
signal_linux_386.go
signal_linux_amd64.go
signal_linux_arm64.go
signal_linux_arm.go
signal_linux_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_linux_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_linux_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_linux_riscv64.go
signal_linux_s390x.go
signal_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_netbsd_386.go
signal_netbsd_amd64.go
signal_netbsd_arm64.go
signal_netbsd_arm.go
signal_netbsd.go
signal_openbsd_386.go
signal_openbsd_amd64.go
signal_openbsd_arm64.go
signal_openbsd_arm.go
signal_openbsd_mips64.go
signal_openbsd.go runtime: switch runtime to libc for openbsd/amd64 2021-01-22 18:58:08 +00:00
signal_plan9.go
signal_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_riscv64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_solaris_amd64.go
signal_solaris.go
signal_unix.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
signal_windows_test.go runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
signal_windows.go runtime: use sigpanic0 on all OSes 2021-04-09 17:49:01 +00:00
sigqueue_note.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sigqueue_plan9.go
sigqueue.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sigtab_aix.go
sigtab_linux_generic.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sigtab_linux_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sizeclasses.go runtime: fix documented alignment of 32KiB and 64KiB size classes 2021-03-13 04:53:32 +00:00
sizeof_test.go
slice_test.go
slice.go
softfloat64_test.go
softfloat64.go
stack_test.go
stack.go cmd/internal/obj/x86: simplify huge frame prologue 2021-04-05 16:22:10 +00:00
string_test.go
string.go runtime: make concatstring{2,3,4,5} consistent w/ compiler's use 2021-04-02 20:26:12 +00:00
stubs2.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs3.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_386.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
stubs_amd64.go reflect: add register ABI support for makeFuncStub and methodValueCall 2021-04-02 16:53:18 +00:00
stubs_arm64.go runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
stubs_arm.go runtime: clean up system calls during cgo callback init 2021-02-19 00:01:25 +00:00
stubs_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_nonlinux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
stubs_s390x.go
stubs.go runtime: port performance-critical functions to regabi 2021-04-12 18:08:47 +00:00
symtab_test.go runtime: non-strict InlTreeIndex lookup in Frames.Next 2021-03-30 15:43:47 +00:00
symtab.go runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
sys_aix_ppc64.s
sys_arm64.go
sys_arm.go
sys_darwin_amd64.s cmd/compile: add clobberdeadreg mode 2021-03-19 23:21:21 +00:00
sys_darwin_arm64.go
sys_darwin_arm64.s
sys_darwin.go runtime: use entersyscall in syscall_syscallX on Darwin 2021-03-01 22:49:36 +00:00
sys_dragonfly_amd64.s runtime: use pipe2 for nonblockingPipe on dragonfly 2021-02-25 18:43:17 +00:00
sys_freebsd_386.s
sys_freebsd_amd64.s
sys_freebsd_arm64.s
sys_freebsd_arm.s
sys_libc.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_linux_386.s
sys_linux_amd64.s cmd/asm,runtime: reduce spellings of GOEXPERIMENTs 2021-04-08 02:17:15 +00:00
sys_linux_arm64.s
sys_linux_arm.s
sys_linux_mips64x.s
sys_linux_mipsx.s
sys_linux_ppc64x.s
sys_linux_riscv64.s
sys_linux_s390x.s
sys_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_mipsx.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_netbsd_386.s runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
sys_netbsd_amd64.s runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
sys_netbsd_arm64.s runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
sys_netbsd_arm.s runtime: fix uses of ABIInternal PCs in assembly 2021-04-01 00:51:26 +00:00
sys_nonppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_openbsd1.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_openbsd2.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_openbsd3.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_openbsd_386.s
sys_openbsd_amd64.s runtime: correct syscall10/syscall10X on openbsd/amd64 2021-01-28 16:02:12 +00:00
sys_openbsd_arm64.s runtime,syscall: convert syscall on openbsd/arm64 to libc 2021-01-28 02:19:23 +00:00
sys_openbsd_arm.s
sys_openbsd_mips64.s
sys_openbsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_plan9_386.s
sys_plan9_amd64.s
sys_plan9_arm.s
sys_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
sys_riscv64.go
sys_s390x.go
sys_solaris_amd64.s
sys_wasm.go runtime: delete gosave (dead code) 2021-02-19 00:41:17 +00:00
sys_wasm.s
sys_windows_386.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
sys_windows_amd64.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
sys_windows_arm64.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
sys_windows_arm.s runtime: eliminate externalthreadhandler 2021-04-13 21:13:12 +00:00
sys_x86.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
syscall2_solaris.go
syscall_aix.go
syscall_solaris.go
syscall_windows_test.go runtime: replace os.MkdirTemp with T.TempDir 2021-04-08 07:33:58 +00:00
syscall_windows.go runtime: support register ABI Go functions from Windows callbacks 2021-03-31 20:09:03 +00:00
textflag.h
time_fake.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
time_nofake.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
time_test.go
time.go runtime, time: disable preemption in addtimer 2021-03-10 21:49:24 +00:00
timeasm.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
timestub2.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
timestub.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
tls_arm64.h runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
tls_arm64.s runtime: convert windows/arm64 assembly 2021-02-19 00:41:03 +00:00
tls_arm.s
tls_mips64x.s
tls_mipsx.s
tls_ppc64x.s cmd/link: support 32b TLS_LE offsets on PPC64 2021-04-13 13:54:51 +00:00
tls_riscv64.s
tls_s390x.s
tls_stub.go runtime: bypass ABI wrapper when calling needm on Windows 2021-03-24 19:18:50 +00:00
tls_windows_amd64.go runtime: bypass ABI wrapper when calling needm on Windows 2021-03-24 19:18:50 +00:00
trace.go runtime: encapsulate access to allgs 2021-03-05 22:09:52 +00:00
traceback.go reflect: add register ABI support for makeFuncStub and methodValueCall 2021-04-02 16:53:18 +00:00
type.go cmd/compile, cmd/link: use weak reference in itab 2021-03-24 14:38:53 +00:00
typekind.go
utf8.go
vdso_elf32.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_elf64.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_freebsd_arm64.go
vdso_freebsd_arm.go
vdso_freebsd_x86.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_freebsd.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_in_none.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_linux_386.go
vdso_linux_amd64.go
vdso_linux_arm64.go
vdso_linux_arm.go
vdso_linux_mips64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_linux_ppc64x.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vdso_linux.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
vlop_386.s
vlop_arm_test.go
vlop_arm.s
vlrt.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
wincallback.go runtime: mark Windows' address-taken asm routines as ABIInternal 2021-03-19 17:08:02 +00:00
write_err_android.go
write_err.go all: go fmt std cmd (but revert vendor) 2021-02-20 03:54:50 +00:00
zcallback_windows_arm64.s runtime: mark Windows' address-taken asm routines as ABIInternal 2021-03-19 17:08:02 +00:00
zcallback_windows_arm.s runtime: mark Windows' address-taken asm routines as ABIInternal 2021-03-19 17:08:02 +00:00
zcallback_windows.go
zcallback_windows.s runtime: mark Windows' address-taken asm routines as ABIInternal 2021-03-19 17:08:02 +00:00