Root Explorer PHP

[ Root System Explorer ]

Editing: write_err_android.go

// Copyright 2014 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

import "unsafe"

var (
	writeHeader = []byte{6 /* ANDROID_LOG_ERROR */, 'G', 'o', 0}
	writePath   = []byte("/dev/log/main\x00")
	writeLogd   = []byte("/dev/socket/logdw\x00")

// guarded by printlock/printunlock.
	writeFD  uintptr
	writeBuf [1024]byte
	writePos int
)

// Prior to Android-L, logging was done through writes to /dev/log files implemented
// in kernel ring buffers. In Android-L, those /dev/log files are no longer
// accessible and logging is done through a centralized user-mode logger, logd.
//
// https://android.googlesource.com/platform/system/core/+/refs/tags/android-6.0.1_r78/liblog/logd_write.c
type loggerType int32

const (
	unknown loggerType = iota
	legacy
	logd
	// TODO(hakim): logging for emulator?
)

var logger loggerType

func writeErr(b []byte) {
	if logger == unknown {
		// Use logd if /dev/socket/logdw is available.
		if v := uintptr(access(&writeLogd[0], 0x02 /* W_OK */)); v == 0 {
			logger = logd
			initLogd()
		} else {
			logger = legacy
			initLegacy()
		}
	}

// Write to stderr for command-line programs.
	write(2, unsafe.Pointer(&b[0]), int32(len(b)))

// Log format: "<header>\x00<message m bytes>\x00"
	//
	// <header>
	//   In legacy mode: "<priority 1 byte><tag n bytes>".
	//   In logd mode: "<android_log_header_t 11 bytes><priority 1 byte><tag n bytes>"
	//
	// The entire log needs to be delivered in a single syscall (the NDK
	// does this with writev). Each log is its own line, so we need to
	// buffer writes until we see a newline.
	var hlen int
	switch logger {
	case logd:
		hlen = writeLogdHeader()
	case legacy:
		hlen = len(writeHeader)
	}

dst := writeBuf[hlen:]
	for _, v := range b {
		if v == 0 { // android logging won't print a zero byte
			v = '0'
		}
		dst[writePos] = v
		writePos++
		if v == '\n' || writePos == len(dst)-1 {
			dst[writePos] = 0
			write(writeFD, unsafe.Pointer(&writeBuf[0]), int32(hlen+writePos))
			for i := range dst {
				dst[i] = 0
			}
			writePos = 0
		}
	}
}

func initLegacy() {
	// In legacy mode, logs are written to /dev/log/main
	writeFD = uintptr(open(&writePath[0], 0x1 /* O_WRONLY */, 0))
	if writeFD == 0 {
		// It is hard to do anything here. Write to stderr just
		// in case user has root on device and has run
		//	adb shell setprop log.redirect-stdio true
		msg := []byte("runtime: cannot open /dev/log/main\x00")
		write(2, unsafe.Pointer(&msg[0]), int32(len(msg)))
		exit(2)
	}

// Prepopulate the invariant header part.
	copy(writeBuf[:len(writeHeader)], writeHeader)
}

// used in initLogdWrite but defined here to avoid heap allocation.
var logdAddr sockaddr_un

func initLogd() {
	// In logd mode, logs are sent to the logd via a unix domain socket.
	logdAddr.family = _AF_UNIX
	copy(logdAddr.path[:], writeLogd)

// We are not using non-blocking I/O because writes taking this path
	// are most likely triggered by panic, we cannot think of the advantage of
	// non-blocking I/O for panic but see disadvantage (dropping panic message),
	// and blocking I/O simplifies the code a lot.
	fd := socket(_AF_UNIX, _SOCK_DGRAM|_O_CLOEXEC, 0)
	if fd < 0 {
		msg := []byte("runtime: cannot create a socket for logging\x00")
		write(2, unsafe.Pointer(&msg[0]), int32(len(msg)))
		exit(2)
	}

errno := connect(fd, unsafe.Pointer(&logdAddr), int32(unsafe.Sizeof(logdAddr)))
	if errno < 0 {
		msg := []byte("runtime: cannot connect to /dev/socket/logdw\x00")
		write(2, unsafe.Pointer(&msg[0]), int32(len(msg)))
		// TODO(hakim): or should we just close fd and hope for better luck next time?
		exit(2)
	}
	writeFD = uintptr(fd)

// Prepopulate invariant part of the header.
	// The first 11 bytes will be populated later in writeLogdHeader.
	copy(writeBuf[11:11+len(writeHeader)], writeHeader)
}

// writeLogdHeader populates the header and returns the length of the payload.
func writeLogdHeader() int {
	hdr := writeBuf[:11]

// The first 11 bytes of the header corresponds to android_log_header_t
	// as defined in system/core/include/private/android_logger.h
	//   hdr[0] log type id (unsigned char), defined in <log/log.h>
	//   hdr[1:2] tid (uint16_t)
	//   hdr[3:11] log_time defined in <log/log_read.h>
	//      hdr[3:7] sec unsigned uint32, little endian.
	//      hdr[7:11] nsec unsigned uint32, little endian.
	hdr[0] = 0 // LOG_ID_MAIN
	sec, nsec, _ := time_now()
	packUint32(hdr[3:7], uint32(sec))
	packUint32(hdr[7:11], uint32(nsec))

// TODO(hakim):  hdr[1:2] = gettid?

return 11 + len(writeHeader)
}

func packUint32(b []byte, v uint32) {
	// little-endian.
	b[0] = byte(v)
	b[1] = byte(v >> 8)
	b[2] = byte(v >> 16)
	b[3] = byte(v >> 24)
}

[ CANCEL ]

Name	Type	Actions
.. (Parent Directory)
📄 HACKING.md	FILE	[EDIT]
📄 Makefile	FILE	[EDIT]
📄 abi_test.go	FILE	[EDIT]
📄 alg.go	FILE	[EDIT]
📄 align_runtime_test.go	FILE	[EDIT]
📄 align_test.go	FILE	[EDIT]
📄 arena.go	FILE	[EDIT]
📄 arena_test.go	FILE	[EDIT]
📁 asan/	DIR
📄 asan.go	FILE	[EDIT]
📄 asan0.go	FILE	[EDIT]
📄 asan_amd64.s	FILE	[EDIT]
📄 asan_arm64.s	FILE	[EDIT]
📄 asan_loong64.s	FILE	[EDIT]
📄 asan_ppc64le.s	FILE	[EDIT]
📄 asan_riscv64.s	FILE	[EDIT]
📄 asm.s	FILE	[EDIT]
📄 asm_386.s	FILE	[EDIT]
📄 asm_amd64.h	FILE	[EDIT]
📄 asm_amd64.s	FILE	[EDIT]
📄 asm_arm.s	FILE	[EDIT]
📄 asm_arm64.s	FILE	[EDIT]
📄 asm_loong64.s	FILE	[EDIT]
📄 asm_mips64x.s	FILE	[EDIT]
📄 asm_mipsx.s	FILE	[EDIT]
📄 asm_ppc64x.h	FILE	[EDIT]
📄 asm_ppc64x.s	FILE	[EDIT]
📄 asm_riscv64.s	FILE	[EDIT]
📄 asm_s390x.s	FILE	[EDIT]
📄 asm_wasm.s	FILE	[EDIT]
📄 atomic_arm64.s	FILE	[EDIT]
📄 atomic_loong64.s	FILE	[EDIT]
📄 atomic_mips64x.s	FILE	[EDIT]
📄 atomic_mipsx.s	FILE	[EDIT]
📄 atomic_pointer.go	FILE	[EDIT]
📄 atomic_ppc64x.s	FILE	[EDIT]
📄 atomic_riscv64.s	FILE	[EDIT]
📄 auxv_none.go	FILE	[EDIT]
📄 callers_test.go	FILE	[EDIT]
📁 cgo/	DIR
📄 cgo.go	FILE	[EDIT]
📄 cgo_mmap.go	FILE	[EDIT]
📄 cgo_ppc64x.go	FILE	[EDIT]
📄 cgo_sigaction.go	FILE	[EDIT]
📄 cgocall.go	FILE	[EDIT]
📄 cgocallback.go	FILE	[EDIT]
📄 cgocheck.go	FILE	[EDIT]
📄 chan.go	FILE	[EDIT]
📄 chan_test.go	FILE	[EDIT]
📄 chanbarrier_test.go	FILE	[EDIT]
📄 checkptr.go	FILE	[EDIT]
📄 checkptr_test.go	FILE	[EDIT]
📄 closure_test.go	FILE	[EDIT]
📄 compiler.go	FILE	[EDIT]
📄 complex.go	FILE	[EDIT]
📄 complex_test.go	FILE	[EDIT]
📄 conv_wasm_test.go	FILE	[EDIT]
📄 coro.go	FILE	[EDIT]
📁 coverage/	DIR
📄 covercounter.go	FILE	[EDIT]
📄 covermeta.go	FILE	[EDIT]
📄 cpuflags.go	FILE	[EDIT]
📄 cpuflags_amd64.go	FILE	[EDIT]
📄 cpuflags_arm64.go	FILE	[EDIT]
📄 cpuprof.go	FILE	[EDIT]
📄 cputicks.go	FILE	[EDIT]
📄 crash_cgo_test.go	FILE	[EDIT]
📄 crash_test.go	FILE	[EDIT]
📄 crash_unix_test.go	FILE	[EDIT]
📄 create_file_nounix.go	FILE	[EDIT]
📄 create_file_unix.go	FILE	[EDIT]
📁 debug/	DIR
📄 debug.go	FILE	[EDIT]
📄 debug_test.go	FILE	[EDIT]
📄 debugcall.go	FILE	[EDIT]
📄 debuglog.go	FILE	[EDIT]
📄 debuglog_off.go	FILE	[EDIT]
📄 debuglog_on.go	FILE	[EDIT]
📄 debuglog_test.go	FILE	[EDIT]
📄 defer_test.go	FILE	[EDIT]
📄 defs1_linux.go	FILE	[EDIT]
📄 defs1_netbsd_386.go	FILE	[EDIT]
📄 defs1_netbsd_amd64.go	FILE	[EDIT]
📄 defs1_netbsd_arm.go	FILE	[EDIT]
📄 defs1_netbsd_arm64.go	FILE	[EDIT]
📄 defs1_solaris_amd64.go	FILE	[EDIT]
📄 defs2_linux.go	FILE	[EDIT]
📄 defs3_linux.go	FILE	[EDIT]
📄 defs_aix.go	FILE	[EDIT]
📄 defs_aix_ppc64.go	FILE	[EDIT]
📄 defs_arm_linux.go	FILE	[EDIT]
📄 defs_darwin.go	FILE	[EDIT]
📄 defs_darwin_amd64.go	FILE	[EDIT]
📄 defs_darwin_arm64.go	FILE	[EDIT]
📄 defs_dragonfly.go	FILE	[EDIT]
📄 defs_dragonfly_amd64.go	FILE	[EDIT]
📄 defs_freebsd.go	FILE	[EDIT]
📄 defs_freebsd_386.go	FILE	[EDIT]
📄 defs_freebsd_amd64.go	FILE	[EDIT]
📄 defs_freebsd_arm.go	FILE	[EDIT]
📄 defs_freebsd_arm64.go	FILE	[EDIT]
📄 defs_freebsd_riscv64.go	FILE	[EDIT]
📄 defs_illumos_amd64.go	FILE	[EDIT]
📄 defs_linux.go	FILE	[EDIT]
📄 defs_linux_386.go	FILE	[EDIT]
📄 defs_linux_amd64.go	FILE	[EDIT]
📄 defs_linux_arm.go	FILE	[EDIT]
📄 defs_linux_arm64.go	FILE	[EDIT]
📄 defs_linux_loong64.go	FILE	[EDIT]
📄 defs_linux_mips64x.go	FILE	[EDIT]
📄 defs_linux_mipsx.go	FILE	[EDIT]
📄 defs_linux_ppc64.go	FILE	[EDIT]
📄 defs_linux_ppc64le.go	FILE	[EDIT]
📄 defs_linux_riscv64.go	FILE	[EDIT]
📄 defs_linux_s390x.go	FILE	[EDIT]
📄 defs_netbsd.go	FILE	[EDIT]
📄 defs_netbsd_386.go	FILE	[EDIT]
📄 defs_netbsd_amd64.go	FILE	[EDIT]
📄 defs_netbsd_arm.go	FILE	[EDIT]
📄 defs_openbsd.go	FILE	[EDIT]
📄 defs_openbsd_386.go	FILE	[EDIT]
📄 defs_openbsd_amd64.go	FILE	[EDIT]
📄 defs_openbsd_arm.go	FILE	[EDIT]
📄 defs_openbsd_arm64.go	FILE	[EDIT]
📄 defs_openbsd_mips64.go	FILE	[EDIT]
📄 defs_openbsd_ppc64.go	FILE	[EDIT]
📄 defs_openbsd_riscv64.go	FILE	[EDIT]
📄 defs_plan9_386.go	FILE	[EDIT]
📄 defs_plan9_amd64.go	FILE	[EDIT]
📄 defs_plan9_arm.go	FILE	[EDIT]
📄 defs_solaris.go	FILE	[EDIT]
📄 defs_solaris_amd64.go	FILE	[EDIT]
📄 defs_windows.go	FILE	[EDIT]
📄 defs_windows_386.go	FILE	[EDIT]
📄 defs_windows_amd64.go	FILE	[EDIT]
📄 defs_windows_arm.go	FILE	[EDIT]
📄 defs_windows_arm64.go	FILE	[EDIT]
📄 duff_386.s	FILE	[EDIT]
📄 duff_amd64.s	FILE	[EDIT]
📄 duff_arm.s	FILE	[EDIT]
📄 duff_arm64.s	FILE	[EDIT]
📄 duff_loong64.s	FILE	[EDIT]
📄 duff_mips64x.s	FILE	[EDIT]
📄 duff_ppc64x.s	FILE	[EDIT]
📄 duff_riscv64.s	FILE	[EDIT]
📄 duff_s390x.s	FILE	[EDIT]
📄 ehooks_test.go	FILE	[EDIT]
📄 env_plan9.go	FILE	[EDIT]
📄 env_posix.go	FILE	[EDIT]
📄 env_test.go	FILE	[EDIT]
📄 error.go	FILE	[EDIT]
📄 example_test.go	FILE	[EDIT]
📄 exithook.go	FILE	[EDIT]
📄 export_aix_test.go	FILE	[EDIT]
📄 export_arm_test.go	FILE	[EDIT]
📄 export_darwin_test.go	FILE	[EDIT]
📄 export_debug_amd64_test.go	FILE	[EDIT]
📄 export_debug_arm64_test.go	FILE	[EDIT]
📄 export_debug_ppc64le_test.go	FILE	[EDIT]
📄 export_debug_test.go	FILE	[EDIT]
📄 export_debuglog_test.go	FILE	[EDIT]
📄 export_linux_test.go	FILE	[EDIT]
📄 export_mmap_test.go	FILE	[EDIT]
📄 export_pipe2_test.go	FILE	[EDIT]
📄 export_pipe_test.go	FILE	[EDIT]
📄 export_test.go	FILE	[EDIT]
📄 export_unix_test.go	FILE	[EDIT]
📄 export_windows_test.go	FILE	[EDIT]
📄 extern.go	FILE	[EDIT]
📄 fastlog2.go	FILE	[EDIT]
📄 fastlog2_test.go	FILE	[EDIT]
📄 fastlog2table.go	FILE	[EDIT]
📄 fds_nonunix.go	FILE	[EDIT]
📄 fds_test.go	FILE	[EDIT]
📄 fds_unix.go	FILE	[EDIT]
📄 float.go	FILE	[EDIT]
📄 float_test.go	FILE	[EDIT]
📄 funcdata.h	FILE	[EDIT]
📄 gc_test.go	FILE	[EDIT]
📄 gcinfo_test.go	FILE	[EDIT]
📄 go_tls.h	FILE	[EDIT]
📄 hash32.go	FILE	[EDIT]
📄 hash64.go	FILE	[EDIT]
📄 hash_test.go	FILE	[EDIT]
📄 heap_test.go	FILE	[EDIT]
📄 heapdump.go	FILE	[EDIT]
📄 histogram.go	FILE	[EDIT]
📄 histogram_test.go	FILE	[EDIT]
📄 iface.go	FILE	[EDIT]
📄 iface_test.go	FILE	[EDIT]
📄 import_test.go	FILE	[EDIT]
📄 importx_test.go	FILE	[EDIT]
📁 internal/	DIR
📄 lfstack.go	FILE	[EDIT]
📄 lfstack_test.go	FILE	[EDIT]
📄 libfuzzer.go	FILE	[EDIT]
📄 libfuzzer_amd64.s	FILE	[EDIT]
📄 libfuzzer_arm64.s	FILE	[EDIT]
📄 lock_futex.go	FILE	[EDIT]
📄 lock_js.go	FILE	[EDIT]
📄 lock_sema.go	FILE	[EDIT]
📄 lock_wasip1.go	FILE	[EDIT]
📄 lockrank.go	FILE	[EDIT]
📄 lockrank_off.go	FILE	[EDIT]
📄 lockrank_on.go	FILE	[EDIT]
📄 lockrank_test.go	FILE	[EDIT]
📄 malloc.go	FILE	[EDIT]
📄 malloc_test.go	FILE	[EDIT]
📄 map.go	FILE	[EDIT]
📄 map_benchmark_test.go	FILE	[EDIT]
📄 map_fast32.go	FILE	[EDIT]
📄 map_fast64.go	FILE	[EDIT]
📄 map_faststr.go	FILE	[EDIT]
📄 map_test.go	FILE	[EDIT]
📄 mbarrier.go	FILE	[EDIT]
📄 mbitmap.go	FILE	[EDIT]
📄 mbitmap_allocheaders.go	FILE	[EDIT]
📄 mbitmap_noallocheaders.go	FILE	[EDIT]
📄 mcache.go	FILE	[EDIT]
📄 mcentral.go	FILE	[EDIT]
📄 mcheckmark.go	FILE	[EDIT]
📄 mem.go	FILE	[EDIT]
📄 mem_aix.go	FILE	[EDIT]
📄 mem_bsd.go	FILE	[EDIT]
📄 mem_darwin.go	FILE	[EDIT]
📄 mem_js.go	FILE	[EDIT]
📄 mem_linux.go	FILE	[EDIT]
📄 mem_plan9.go	FILE	[EDIT]
📄 mem_sbrk.go	FILE	[EDIT]
📄 mem_wasip1.go	FILE	[EDIT]
📄 mem_wasm.go	FILE	[EDIT]
📄 mem_windows.go	FILE	[EDIT]
📄 memclr_386.s	FILE	[EDIT]
📄 memclr_amd64.s	FILE	[EDIT]
📄 memclr_arm.s	FILE	[EDIT]
📄 memclr_arm64.s	FILE	[EDIT]
📄 memclr_loong64.s	FILE	[EDIT]
📄 memclr_mips64x.s	FILE	[EDIT]
📄 memclr_mipsx.s	FILE	[EDIT]
📄 memclr_plan9_386.s	FILE	[EDIT]
📄 memclr_plan9_amd64.s	FILE	[EDIT]
📄 memclr_ppc64x.s	FILE	[EDIT]
📄 memclr_riscv64.s	FILE	[EDIT]
📄 memclr_s390x.s	FILE	[EDIT]
📄 memclr_wasm.s	FILE	[EDIT]
📄 memmove_386.s	FILE	[EDIT]
📄 memmove_amd64.s	FILE	[EDIT]
📄 memmove_arm.s	FILE	[EDIT]
📄 memmove_arm64.s	FILE	[EDIT]
📄 memmove_linux_amd64_test.go	FILE	[EDIT]
📄 memmove_loong64.s	FILE	[EDIT]
📄 memmove_mips64x.s	FILE	[EDIT]
📄 memmove_mipsx.s	FILE	[EDIT]
📄 memmove_plan9_386.s	FILE	[EDIT]
📄 memmove_plan9_amd64.s	FILE	[EDIT]
📄 memmove_ppc64x.s	FILE	[EDIT]
📄 memmove_riscv64.s	FILE	[EDIT]
📄 memmove_s390x.s	FILE	[EDIT]
📄 memmove_test.go	FILE	[EDIT]
📄 memmove_wasm.s	FILE	[EDIT]
📁 metrics/	DIR
📄 metrics.go	FILE	[EDIT]
📄 metrics_test.go	FILE	[EDIT]
📄 mfinal.go	FILE	[EDIT]
📄 mfinal_test.go	FILE	[EDIT]
📄 mfixalloc.go	FILE	[EDIT]
📄 mgc.go	FILE	[EDIT]
📄 mgclimit.go	FILE	[EDIT]
📄 mgclimit_test.go	FILE	[EDIT]
📄 mgcmark.go	FILE	[EDIT]
📄 mgcpacer.go	FILE	[EDIT]
📄 mgcpacer_test.go	FILE	[EDIT]
📄 mgcscavenge.go	FILE	[EDIT]
📄 mgcscavenge_test.go	FILE	[EDIT]
📄 mgcstack.go	FILE	[EDIT]
📄 mgcsweep.go	FILE	[EDIT]
📄 mgcwork.go	FILE	[EDIT]
📄 mheap.go	FILE	[EDIT]
📄 minmax.go	FILE	[EDIT]
📄 minmax_test.go	FILE	[EDIT]
📄 mkduff.go	FILE	[EDIT]
📄 mkfastlog2table.go	FILE	[EDIT]
📄 mklockrank.go	FILE	[EDIT]
📄 mkpreempt.go	FILE	[EDIT]
📄 mksizeclasses.go	FILE	[EDIT]
📄 mmap.go	FILE	[EDIT]
📄 mpagealloc.go	FILE	[EDIT]
📄 mpagealloc_32bit.go	FILE	[EDIT]
📄 mpagealloc_64bit.go	FILE	[EDIT]
📄 mpagealloc_test.go	FILE	[EDIT]
📄 mpagecache.go	FILE	[EDIT]
📄 mpagecache_test.go	FILE	[EDIT]
📄 mpallocbits.go	FILE	[EDIT]
📄 mpallocbits_test.go	FILE	[EDIT]
📄 mprof.go	FILE	[EDIT]
📄 mranges.go	FILE	[EDIT]
📄 mranges_test.go	FILE	[EDIT]
📁 msan/	DIR
📄 msan.go	FILE	[EDIT]
📄 msan0.go	FILE	[EDIT]
📄 msan_amd64.s	FILE	[EDIT]
📄 msan_arm64.s	FILE	[EDIT]
📄 msan_loong64.s	FILE	[EDIT]
📄 msize_allocheaders.go	FILE	[EDIT]
📄 msize_noallocheaders.go	FILE	[EDIT]
📄 mspanset.go	FILE	[EDIT]
📄 mstats.go	FILE	[EDIT]
📄 mwbbuf.go	FILE	[EDIT]
📄 nbpipe_pipe.go	FILE	[EDIT]
📄 nbpipe_pipe2.go	FILE	[EDIT]
📄 nbpipe_pipe_test.go	FILE	[EDIT]
📄 nbpipe_test.go	FILE	[EDIT]
📄 net_plan9.go	FILE	[EDIT]
📄 netpoll.go	FILE	[EDIT]
📄 netpoll_aix.go	FILE	[EDIT]
📄 netpoll_epoll.go	FILE	[EDIT]
📄 netpoll_fake.go	FILE	[EDIT]
📄 netpoll_kqueue.go	FILE	[EDIT]
📄 netpoll_os_test.go	FILE	[EDIT]
📄 netpoll_solaris.go	FILE	[EDIT]
📄 netpoll_stub.go	FILE	[EDIT]
📄 netpoll_wasip1.go	FILE	[EDIT]
📄 netpoll_windows.go	FILE	[EDIT]
📄 nonwindows_stub.go	FILE	[EDIT]
📄 norace_linux_test.go	FILE	[EDIT]
📄 norace_test.go	FILE	[EDIT]
📄 numcpu_freebsd_test.go	FILE	[EDIT]
📄 os2_aix.go	FILE	[EDIT]
📄 os2_freebsd.go	FILE	[EDIT]
📄 os2_openbsd.go	FILE	[EDIT]
📄 os2_plan9.go	FILE	[EDIT]
📄 os2_solaris.go	FILE	[EDIT]
📄 os3_plan9.go	FILE	[EDIT]
📄 os3_solaris.go	FILE	[EDIT]
📄 os_aix.go	FILE	[EDIT]
📄 os_android.go	FILE	[EDIT]
📄 os_darwin.go	FILE	[EDIT]
📄 os_darwin_arm64.go	FILE	[EDIT]
📄 os_dragonfly.go	FILE	[EDIT]
📄 os_freebsd.go	FILE	[EDIT]
📄 os_freebsd2.go	FILE	[EDIT]
📄 os_freebsd_amd64.go	FILE	[EDIT]
📄 os_freebsd_arm.go	FILE	[EDIT]
📄 os_freebsd_arm64.go	FILE	[EDIT]
📄 os_freebsd_noauxv.go	FILE	[EDIT]
📄 os_freebsd_riscv64.go	FILE	[EDIT]
📄 os_illumos.go	FILE	[EDIT]
📄 os_js.go	FILE	[EDIT]
📄 os_linux.go	FILE	[EDIT]
📄 os_linux_arm.go	FILE	[EDIT]
📄 os_linux_arm64.go	FILE	[EDIT]
📄 os_linux_be64.go	FILE	[EDIT]
📄 os_linux_generic.go	FILE	[EDIT]
📄 os_linux_loong64.go	FILE	[EDIT]
📄 os_linux_mips64x.go	FILE	[EDIT]
📄 os_linux_mipsx.go	FILE	[EDIT]
📄 os_linux_noauxv.go	FILE	[EDIT]
📄 os_linux_novdso.go	FILE	[EDIT]
📄 os_linux_ppc64x.go	FILE	[EDIT]
📄 os_linux_riscv64.go	FILE	[EDIT]
📄 os_linux_s390x.go	FILE	[EDIT]
📄 os_linux_x86.go	FILE	[EDIT]
📄 os_netbsd.go	FILE	[EDIT]
📄 os_netbsd_386.go	FILE	[EDIT]
📄 os_netbsd_amd64.go	FILE	[EDIT]
📄 os_netbsd_arm.go	FILE	[EDIT]
📄 os_netbsd_arm64.go	FILE	[EDIT]
📄 os_nonopenbsd.go	FILE	[EDIT]
📄 os_only_solaris.go	FILE	[EDIT]
📄 os_openbsd.go	FILE	[EDIT]
📄 os_openbsd_arm.go	FILE	[EDIT]
📄 os_openbsd_arm64.go	FILE	[EDIT]
📄 os_openbsd_libc.go	FILE	[EDIT]
📄 os_openbsd_mips64.go	FILE	[EDIT]
📄 os_openbsd_syscall.go	FILE	[EDIT]
📄 os_openbsd_syscall1.go	FILE	[EDIT]
📄 os_openbsd_syscall2.go	FILE	[EDIT]
📄 os_plan9.go	FILE	[EDIT]
📄 os_plan9_arm.go	FILE	[EDIT]
📄 os_solaris.go	FILE	[EDIT]
📄 os_unix.go	FILE	[EDIT]
📄 os_unix_nonlinux.go	FILE	[EDIT]
📄 os_wasip1.go	FILE	[EDIT]
📄 os_wasm.go	FILE	[EDIT]
📄 os_windows.go	FILE	[EDIT]
📄 os_windows_arm.go	FILE	[EDIT]
📄 os_windows_arm64.go	FILE	[EDIT]
📄 pagetrace_off.go	FILE	[EDIT]
📄 pagetrace_on.go	FILE	[EDIT]
📄 panic.go	FILE	[EDIT]
📄 panic32.go	FILE	[EDIT]
📄 panic_test.go	FILE	[EDIT]
📄 panicnil_test.go	FILE	[EDIT]
📄 pinner.go	FILE	[EDIT]
📄 pinner_test.go	FILE	[EDIT]
📄 plugin.go	FILE	[EDIT]
📁 pprof/	DIR
📄 preempt.go	FILE	[EDIT]
📄 preempt_386.s	FILE	[EDIT]
📄 preempt_amd64.s	FILE	[EDIT]
📄 preempt_arm.s	FILE	[EDIT]
📄 preempt_arm64.s	FILE	[EDIT]
📄 preempt_loong64.s	FILE	[EDIT]
📄 preempt_mips64x.s	FILE	[EDIT]
📄 preempt_mipsx.s	FILE	[EDIT]
📄 preempt_nonwindows.go	FILE	[EDIT]
📄 preempt_ppc64x.s	FILE	[EDIT]
📄 preempt_riscv64.s	FILE	[EDIT]
📄 preempt_s390x.s	FILE	[EDIT]
📄 preempt_wasm.s	FILE	[EDIT]
📄 print.go	FILE	[EDIT]
📄 proc.go	FILE	[EDIT]
📄 proc_runtime_test.go	FILE	[EDIT]
📄 proc_test.go	FILE	[EDIT]
📄 profbuf.go	FILE	[EDIT]
📄 profbuf_test.go	FILE	[EDIT]
📄 proflabel.go	FILE	[EDIT]
📁 race/	DIR
📄 race.go	FILE	[EDIT]
📄 race0.go	FILE	[EDIT]
📄 race_amd64.s	FILE	[EDIT]
📄 race_arm64.s	FILE	[EDIT]
📄 race_ppc64le.s	FILE	[EDIT]
📄 race_s390x.s	FILE	[EDIT]
📄 rand.go	FILE	[EDIT]
📄 rand_test.go	FILE	[EDIT]
📄 rdebug.go	FILE	[EDIT]
📄 retry.go	FILE	[EDIT]
📄 rt0_aix_ppc64.s	FILE	[EDIT]
📄 rt0_android_386.s	FILE	[EDIT]
📄 rt0_android_amd64.s	FILE	[EDIT]
📄 rt0_android_arm.s	FILE	[EDIT]
📄 rt0_android_arm64.s	FILE	[EDIT]
📄 rt0_darwin_amd64.s	FILE	[EDIT]
📄 rt0_darwin_arm64.s	FILE	[EDIT]
📄 rt0_dragonfly_amd64.s	FILE	[EDIT]
📄 rt0_freebsd_386.s	FILE	[EDIT]
📄 rt0_freebsd_amd64.s	FILE	[EDIT]
📄 rt0_freebsd_arm.s	FILE	[EDIT]
📄 rt0_freebsd_arm64.s	FILE	[EDIT]
📄 rt0_freebsd_riscv64.s	FILE	[EDIT]
📄 rt0_illumos_amd64.s	FILE	[EDIT]
📄 rt0_ios_amd64.s	FILE	[EDIT]
📄 rt0_ios_arm64.s	FILE	[EDIT]
📄 rt0_js_wasm.s	FILE	[EDIT]
📄 rt0_linux_386.s	FILE	[EDIT]
📄 rt0_linux_amd64.s	FILE	[EDIT]
📄 rt0_linux_arm.s	FILE	[EDIT]
📄 rt0_linux_arm64.s	FILE	[EDIT]
📄 rt0_linux_loong64.s	FILE	[EDIT]
📄 rt0_linux_mips64x.s	FILE	[EDIT]
📄 rt0_linux_mipsx.s	FILE	[EDIT]
📄 rt0_linux_ppc64.s	FILE	[EDIT]
📄 rt0_linux_ppc64le.s	FILE	[EDIT]
📄 rt0_linux_riscv64.s	FILE	[EDIT]
📄 rt0_linux_s390x.s	FILE	[EDIT]
📄 rt0_netbsd_386.s	FILE	[EDIT]
📄 rt0_netbsd_amd64.s	FILE	[EDIT]
📄 rt0_netbsd_arm.s	FILE	[EDIT]
📄 rt0_netbsd_arm64.s	FILE	[EDIT]
📄 rt0_openbsd_386.s	FILE	[EDIT]
📄 rt0_openbsd_amd64.s	FILE	[EDIT]
📄 rt0_openbsd_arm.s	FILE	[EDIT]
📄 rt0_openbsd_arm64.s	FILE	[EDIT]
📄 rt0_openbsd_mips64.s	FILE	[EDIT]
📄 rt0_openbsd_ppc64.s	FILE	[EDIT]
📄 rt0_openbsd_riscv64.s	FILE	[EDIT]
📄 rt0_plan9_386.s	FILE	[EDIT]
📄 rt0_plan9_amd64.s	FILE	[EDIT]
📄 rt0_plan9_arm.s	FILE	[EDIT]
📄 rt0_solaris_amd64.s	FILE	[EDIT]
📄 rt0_wasip1_wasm.s	FILE	[EDIT]
📄 rt0_windows_386.s	FILE	[EDIT]
📄 rt0_windows_amd64.s	FILE	[EDIT]
📄 rt0_windows_arm.s	FILE	[EDIT]
📄 rt0_windows_arm64.s	FILE	[EDIT]
📄 runtime-gdb.py	FILE	[EDIT]
📄 runtime-gdb_test.go	FILE	[EDIT]
📄 runtime-gdb_unix_test.go	FILE	[EDIT]
📄 runtime-lldb_test.go	FILE	[EDIT]
📄 runtime-seh_windows_test.go	FILE	[EDIT]
📄 runtime.go	FILE	[EDIT]
📄 runtime1.go	FILE	[EDIT]
📄 runtime2.go	FILE	[EDIT]
📄 runtime_boring.go	FILE	[EDIT]
📄 runtime_linux_test.go	FILE	[EDIT]
📄 runtime_mmap_test.go	FILE	[EDIT]
📄 runtime_test.go	FILE	[EDIT]
📄 runtime_unix_test.go	FILE	[EDIT]
📄 rwmutex.go	FILE	[EDIT]
📄 rwmutex_test.go	FILE	[EDIT]
📄 security_aix.go	FILE	[EDIT]
📄 security_issetugid.go	FILE	[EDIT]
📄 security_linux.go	FILE	[EDIT]
📄 security_nonunix.go	FILE	[EDIT]
📄 security_test.go	FILE	[EDIT]
📄 security_unix.go	FILE	[EDIT]
📄 select.go	FILE	[EDIT]
📄 sema.go	FILE	[EDIT]
📄 sema_test.go	FILE	[EDIT]
📄 semasleep_test.go	FILE	[EDIT]
📄 sigaction.go	FILE	[EDIT]
📄 signal_386.go	FILE	[EDIT]
📄 signal_aix_ppc64.go	FILE	[EDIT]
📄 signal_amd64.go	FILE	[EDIT]
📄 signal_arm.go	FILE	[EDIT]
📄 signal_arm64.go	FILE	[EDIT]
📄 signal_darwin.go	FILE	[EDIT]
📄 signal_darwin_amd64.go	FILE	[EDIT]
📄 signal_darwin_arm64.go	FILE	[EDIT]
📄 signal_dragonfly.go	FILE	[EDIT]
📄 signal_dragonfly_amd64.go	FILE	[EDIT]
📄 signal_freebsd.go	FILE	[EDIT]
📄 signal_freebsd_386.go	FILE	[EDIT]
📄 signal_freebsd_amd64.go	FILE	[EDIT]
📄 signal_freebsd_arm.go	FILE	[EDIT]
📄 signal_freebsd_arm64.go	FILE	[EDIT]
📄 signal_freebsd_riscv64.go	FILE	[EDIT]
📄 signal_linux_386.go	FILE	[EDIT]
📄 signal_linux_amd64.go	FILE	[EDIT]
📄 signal_linux_arm.go	FILE	[EDIT]
📄 signal_linux_arm64.go	FILE	[EDIT]
📄 signal_linux_loong64.go	FILE	[EDIT]
📄 signal_linux_mips64x.go	FILE	[EDIT]
📄 signal_linux_mipsx.go	FILE	[EDIT]
📄 signal_linux_ppc64x.go	FILE	[EDIT]
📄 signal_linux_riscv64.go	FILE	[EDIT]
📄 signal_linux_s390x.go	FILE	[EDIT]
📄 signal_loong64.go	FILE	[EDIT]
📄 signal_mips64x.go	FILE	[EDIT]
📄 signal_mipsx.go	FILE	[EDIT]
📄 signal_netbsd.go	FILE	[EDIT]
📄 signal_netbsd_386.go	FILE	[EDIT]
📄 signal_netbsd_amd64.go	FILE	[EDIT]
📄 signal_netbsd_arm.go	FILE	[EDIT]
📄 signal_netbsd_arm64.go	FILE	[EDIT]
📄 signal_openbsd.go	FILE	[EDIT]
📄 signal_openbsd_386.go	FILE	[EDIT]
📄 signal_openbsd_amd64.go	FILE	[EDIT]
📄 signal_openbsd_arm.go	FILE	[EDIT]
📄 signal_openbsd_arm64.go	FILE	[EDIT]
📄 signal_openbsd_mips64.go	FILE	[EDIT]
📄 signal_openbsd_ppc64.go	FILE	[EDIT]
📄 signal_openbsd_riscv64.go	FILE	[EDIT]
📄 signal_plan9.go	FILE	[EDIT]
📄 signal_ppc64x.go	FILE	[EDIT]
📄 signal_riscv64.go	FILE	[EDIT]
📄 signal_solaris.go	FILE	[EDIT]
📄 signal_solaris_amd64.go	FILE	[EDIT]
📄 signal_unix.go	FILE	[EDIT]
📄 signal_windows.go	FILE	[EDIT]
📄 signal_windows_test.go	FILE	[EDIT]
📄 sigqueue.go	FILE	[EDIT]
📄 sigqueue_note.go	FILE	[EDIT]
📄 sigqueue_plan9.go	FILE	[EDIT]
📄 sigtab_aix.go	FILE	[EDIT]
📄 sigtab_linux_generic.go	FILE	[EDIT]
📄 sigtab_linux_mipsx.go	FILE	[EDIT]
📄 sizeclasses.go	FILE	[EDIT]
📄 sizeof_test.go	FILE	[EDIT]
📄 slice.go	FILE	[EDIT]
📄 slice_test.go	FILE	[EDIT]
📄 softfloat64.go	FILE	[EDIT]
📄 softfloat64_test.go	FILE	[EDIT]
📄 stack.go	FILE	[EDIT]
📄 stack_test.go	FILE	[EDIT]
📄 start_line_amd64_test.go	FILE	[EDIT]
📄 start_line_test.go	FILE	[EDIT]
📄 stkframe.go	FILE	[EDIT]
📄 string.go	FILE	[EDIT]
📄 string_test.go	FILE	[EDIT]
📄 stubs.go	FILE	[EDIT]
📄 stubs2.go	FILE	[EDIT]
📄 stubs3.go	FILE	[EDIT]
📄 stubs_386.go	FILE	[EDIT]
📄 stubs_amd64.go	FILE	[EDIT]
📄 stubs_arm.go	FILE	[EDIT]
📄 stubs_arm64.go	FILE	[EDIT]
📄 stubs_linux.go	FILE	[EDIT]
📄 stubs_loong64.go	FILE	[EDIT]
📄 stubs_mips64x.go	FILE	[EDIT]
📄 stubs_mipsx.go	FILE	[EDIT]
📄 stubs_nonlinux.go	FILE	[EDIT]
📄 stubs_ppc64.go	FILE	[EDIT]
📄 stubs_ppc64x.go	FILE	[EDIT]
📄 stubs_riscv64.go	FILE	[EDIT]
📄 stubs_s390x.go	FILE	[EDIT]
📄 symtab.go	FILE	[EDIT]
📄 symtab_test.go	FILE	[EDIT]
📄 symtabinl.go	FILE	[EDIT]
📄 symtabinl_test.go	FILE	[EDIT]
📄 sys_aix_ppc64.s	FILE	[EDIT]
📄 sys_arm.go	FILE	[EDIT]
📄 sys_arm64.go	FILE	[EDIT]
📄 sys_darwin.go	FILE	[EDIT]
📄 sys_darwin_amd64.s	FILE	[EDIT]
📄 sys_darwin_arm64.go	FILE	[EDIT]
📄 sys_darwin_arm64.s	FILE	[EDIT]
📄 sys_dragonfly_amd64.s	FILE	[EDIT]
📄 sys_freebsd_386.s	FILE	[EDIT]
📄 sys_freebsd_amd64.s	FILE	[EDIT]
📄 sys_freebsd_arm.s	FILE	[EDIT]
📄 sys_freebsd_arm64.s	FILE	[EDIT]
📄 sys_freebsd_riscv64.s	FILE	[EDIT]
📄 sys_libc.go	FILE	[EDIT]
📄 sys_linux_386.s	FILE	[EDIT]
📄 sys_linux_amd64.s	FILE	[EDIT]
📄 sys_linux_arm.s	FILE	[EDIT]
📄 sys_linux_arm64.s	FILE	[EDIT]
📄 sys_linux_loong64.s	FILE	[EDIT]
📄 sys_linux_mips64x.s	FILE	[EDIT]
📄 sys_linux_mipsx.s	FILE	[EDIT]
📄 sys_linux_ppc64x.s	FILE	[EDIT]
📄 sys_linux_riscv64.s	FILE	[EDIT]
📄 sys_linux_s390x.s	FILE	[EDIT]
📄 sys_loong64.go	FILE	[EDIT]
📄 sys_mips64x.go	FILE	[EDIT]
📄 sys_mipsx.go	FILE	[EDIT]
📄 sys_netbsd_386.s	FILE	[EDIT]
📄 sys_netbsd_amd64.s	FILE	[EDIT]
📄 sys_netbsd_arm.s	FILE	[EDIT]
📄 sys_netbsd_arm64.s	FILE	[EDIT]
📄 sys_nonppc64x.go	FILE	[EDIT]
📄 sys_openbsd.go	FILE	[EDIT]
📄 sys_openbsd1.go	FILE	[EDIT]
📄 sys_openbsd2.go	FILE	[EDIT]
📄 sys_openbsd3.go	FILE	[EDIT]
📄 sys_openbsd_386.s	FILE	[EDIT]
📄 sys_openbsd_amd64.s	FILE	[EDIT]
📄 sys_openbsd_arm.s	FILE	[EDIT]
📄 sys_openbsd_arm64.s	FILE	[EDIT]
📄 sys_openbsd_mips64.s	FILE	[EDIT]
📄 sys_openbsd_ppc64.s	FILE	[EDIT]
📄 sys_openbsd_riscv64.s	FILE	[EDIT]
📄 sys_plan9_386.s	FILE	[EDIT]
📄 sys_plan9_amd64.s	FILE	[EDIT]
📄 sys_plan9_arm.s	FILE	[EDIT]
📄 sys_ppc64x.go	FILE	[EDIT]
📄 sys_riscv64.go	FILE	[EDIT]
📄 sys_s390x.go	FILE	[EDIT]
📄 sys_solaris_amd64.s	FILE	[EDIT]
📄 sys_wasm.go	FILE	[EDIT]
📄 sys_wasm.s	FILE	[EDIT]
📄 sys_windows_386.s	FILE	[EDIT]
📄 sys_windows_amd64.s	FILE	[EDIT]
📄 sys_windows_arm.s	FILE	[EDIT]
📄 sys_windows_arm64.s	FILE	[EDIT]
📄 sys_x86.go	FILE	[EDIT]
📄 syscall2_solaris.go	FILE	[EDIT]
📄 syscall_aix.go	FILE	[EDIT]
📄 syscall_solaris.go	FILE	[EDIT]
📄 syscall_unix_test.go	FILE	[EDIT]
📄 syscall_windows.go	FILE	[EDIT]
📄 syscall_windows_test.go	FILE	[EDIT]
📄 tagptr.go	FILE	[EDIT]
📄 tagptr_32bit.go	FILE	[EDIT]
📄 tagptr_64bit.go	FILE	[EDIT]
📄 test_amd64.go	FILE	[EDIT]
📄 test_amd64.s	FILE	[EDIT]
📄 test_stubs.go	FILE	[EDIT]
📁 testdata/	DIR
📄 textflag.h	FILE	[EDIT]
📄 time.go	FILE	[EDIT]
📄 time_fake.go	FILE	[EDIT]
📄 time_linux_amd64.s	FILE	[EDIT]
📄 time_nofake.go	FILE	[EDIT]
📄 time_test.go	FILE	[EDIT]
📄 time_windows.h	FILE	[EDIT]
📄 time_windows_386.s	FILE	[EDIT]
📄 time_windows_amd64.s	FILE	[EDIT]
📄 time_windows_arm.s	FILE	[EDIT]
📄 time_windows_arm64.s	FILE	[EDIT]
📄 timeasm.go	FILE	[EDIT]
📄 timestub.go	FILE	[EDIT]
📄 timestub2.go	FILE	[EDIT]
📄 tls_arm.s	FILE	[EDIT]
📄 tls_arm64.h	FILE	[EDIT]
📄 tls_arm64.s	FILE	[EDIT]
📄 tls_loong64.s	FILE	[EDIT]
📄 tls_mips64x.s	FILE	[EDIT]
📄 tls_mipsx.s	FILE	[EDIT]
📄 tls_ppc64x.s	FILE	[EDIT]
📄 tls_riscv64.s	FILE	[EDIT]
📄 tls_s390x.s	FILE	[EDIT]
📄 tls_stub.go	FILE	[EDIT]
📄 tls_windows_amd64.go	FILE	[EDIT]
📁 trace/	DIR
📄 trace.go	FILE	[EDIT]
📄 trace2.go	FILE	[EDIT]
📄 trace2buf.go	FILE	[EDIT]
📄 trace2cpu.go	FILE	[EDIT]
📄 trace2event.go	FILE	[EDIT]
📄 trace2map.go	FILE	[EDIT]
📄 trace2region.go	FILE	[EDIT]
📄 trace2runtime.go	FILE	[EDIT]
📄 trace2stack.go	FILE	[EDIT]
📄 trace2status.go	FILE	[EDIT]
📄 trace2string.go	FILE	[EDIT]
📄 trace2time.go	FILE	[EDIT]
📄 trace_cgo_test.go	FILE	[EDIT]
📄 traceback.go	FILE	[EDIT]
📄 traceback_test.go	FILE	[EDIT]
📄 tracebackx_test.go	FILE	[EDIT]
📄 type.go	FILE	[EDIT]
📄 typekind.go	FILE	[EDIT]
📄 unsafe.go	FILE	[EDIT]
📄 unsafepoint_test.go	FILE	[EDIT]
📄 utf8.go	FILE	[EDIT]
📄 vdso_elf32.go	FILE	[EDIT]
📄 vdso_elf64.go	FILE	[EDIT]
📄 vdso_freebsd.go	FILE	[EDIT]
📄 vdso_freebsd_arm.go	FILE	[EDIT]
📄 vdso_freebsd_arm64.go	FILE	[EDIT]
📄 vdso_freebsd_riscv64.go	FILE	[EDIT]
📄 vdso_freebsd_x86.go	FILE	[EDIT]
📄 vdso_in_none.go	FILE	[EDIT]
📄 vdso_linux.go	FILE	[EDIT]
📄 vdso_linux_386.go	FILE	[EDIT]
📄 vdso_linux_amd64.go	FILE	[EDIT]
📄 vdso_linux_arm.go	FILE	[EDIT]
📄 vdso_linux_arm64.go	FILE	[EDIT]
📄 vdso_linux_loong64.go	FILE	[EDIT]
📄 vdso_linux_mips64x.go	FILE	[EDIT]
📄 vdso_linux_ppc64x.go	FILE	[EDIT]
📄 vdso_linux_riscv64.go	FILE	[EDIT]
📄 vdso_linux_s390x.go	FILE	[EDIT]
📄 vdso_test.go	FILE	[EDIT]
📄 vlop_386.s	FILE	[EDIT]
📄 vlop_arm.s	FILE	[EDIT]
📄 vlop_arm_test.go	FILE	[EDIT]
📄 vlrt.go	FILE	[EDIT]
📄 wincallback.go	FILE	[EDIT]
📄 write_err.go	FILE	[EDIT]
📄 write_err_android.go	FILE	[EDIT]
📄 zcallback_windows.go	FILE	[EDIT]
📄 zcallback_windows.s	FILE	[EDIT]
📄 zcallback_windows_arm.s	FILE	[EDIT]
📄 zcallback_windows_arm64.s	FILE	[EDIT]