OpenE2K/gcc
2
0
Fork 0
Code Issues Pull Requests Projects Releases Wiki Activity
gcc/libgo/go/runtime
History
Lynn Boger 2fbed0dc6c libgo: ensure memmove, memset 8 byte atomicity on ppc64x 
Go requires that pointer moves are done 8 bytes at a time,
but gccgo uses libc's memmove and memset which does not require
that, and there are some cases where an 8 byte move might be
done as 4+4.

To enforce 8 byte moves for memmove and memset, this adds a
C implementation in libgo/runtime for memmove and memset to be
used on ppc64le and ppc64. Asm implementations were considered
but discarded to avoid different implementations for different
target ISAs.

Fixes golang/go#41428

Reviewed-on: https://go-review.googlesource.com/c/gofrontend/+/294931
2021-02-25 17:01:23 -08:00
..
debug
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
internal
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
metrics
libgo: update to Go1.16 release
2021-02-19 12:33:25 -08:00
msan
…
pprof
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
testdata
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
trace
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
alg.go
runtime: revert eqtype for AIX
2020-08-10 16:45:16 -07:00
atomic_pointer.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
auxv_none.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
callers_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
cgo_gccgo.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
cgocall.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
cgocheck.go
compiler,runtime: pass only ptr and len to some runtime calls
2020-07-27 17:05:17 -07:00
chan_test.go
libgo: update to Go 1.15.3 release
2020-10-27 13:58:02 -07:00
chan.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
chanbarrier_test.go
…
checkptr_test.go
libgo: update to Go1.15.2 release
2020-09-23 17:32:49 -07:00
checkptr.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
closure_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
compiler.go
…
complex_test.go
…
conv_wasm_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
cpuflags_arm64.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
cpuprof.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
cputicks.go
…
crash_cgo_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
crash_gccgo_test.go
…
crash_nonunix_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
crash_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
crash_unix_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
debug_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
debug.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
debuglog_off.go
…
debuglog_on.go
…
debuglog_test.go
…
debuglog.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
defer_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
env_posix.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
env_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
eqtype_aix_gccgo.go
runtime: revert eqtype for AIX
2020-08-10 16:45:16 -07:00
eqtype.go
runtime: revert eqtype for AIX
2020-08-10 16:45:16 -07:00
error.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
example_test.go
…
export_debug_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
export_debuglog_test.go
…
export_linux_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
export_mmap_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
export_pipe2_test.go
libgo: update hurd support
2021-01-14 09:57:04 -08:00
export_pipe_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
export_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
export_unix_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
export_windows_test.go
…
extern.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
fastlog2_test.go
…
fastlog2.go
…
fastlog2table.go
…
ffi.go
…
float.go
…
gc_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
gcinfo_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
hash32.go
libgo: add 32-bit RISC-V (RV32) support
2020-09-30 19:47:48 -07:00
hash64.go
libgo: update to Go1.14rc1 release
2020-02-15 09:14:10 -08:00
hash_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
heapdump.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
histogram_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
histogram.go
libgo: update to Go1.16 release
2021-02-19 12:33:25 -08:00
iface_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
iface.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
lfstack_32bit.go
libgo: add 32-bit RISC-V (RV32) support
2020-09-30 19:47:48 -07:00
lfstack_64bit.go
libgo: update to Go1.14rc1 release
2020-02-15 09:14:10 -08:00
lfstack_test.go
…
lfstack.go
…
libfuzzer.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
lock_futex.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
lock_js.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
lock_sema.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
lockrank_off.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
lockrank_on.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
lockrank.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
malloc_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
malloc.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map_benchmark_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map_fast32.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map_fast64.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map_faststr.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
map.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mbarrier.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mbitmap.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mcache.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mcentral.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mcheckmark.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mem_gccgo.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
memmove_linux_amd64_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
memmove_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
metrics_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
metrics.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
mfinal_test.go
…
mfinal.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mfixalloc.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mgc_gccgo.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
mgc.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mgcmark.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
mgcscavenge_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mgcscavenge.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
mgcsweep.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mgcwork.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mheap.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mkfastlog2table.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mkpreempt.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mksizeclasses.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpagealloc_32bit.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpagealloc_64bit.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpagealloc_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpagealloc.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpagecache_test.go
libgo: update to Go 1.14.4 release
2020-07-10 11:30:23 -07:00
mpagecache.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpallocbits_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mpallocbits.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mprof.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
mranges_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mranges.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
msan0.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
msize.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
mspanset.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mstats.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
mwbbuf.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
nbpipe_pipe2.go
runtime, syscall: add a couple of hurd build tags
2020-01-29 16:43:57 -08:00
nbpipe_pipe.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
nbpipe_test.go
libgo: update hurd support
2021-01-14 09:57:04 -08:00
net_plan9.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
netpoll_aix.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll_epoll.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll_fake.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
netpoll_hurd.go
runtime: update netpoll_hurd.go for go1.14beta1 changes
2020-01-29 16:40:19 -08:00
netpoll_kqueue.go
libgo: handle linking to NetBSD's versioned symbols
2020-10-28 18:20:50 -07:00
netpoll_os_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll_solaris.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll_stub.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll_windows.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
netpoll.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
norace_test.go
…
numcpu_freebsd_test.go
…
os3_solaris.go
runtime: for Solaris, add osinit, and drop duplicate getncpu
2020-01-22 15:08:25 -08:00
os_aix.go
internal/cpu: correctly link to getsystemcfg
2021-01-29 16:12:43 -08:00
os_darwin.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_dragonfly.go
…
os_freebsd_arm64.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
os_freebsd.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
os_gccgo.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
os_hurd.go
libgo: update hurd support
2021-01-14 09:57:04 -08:00
os_illumos.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_js.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
os_linux_arm64.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
os_linux_arm.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_linux_mips64x.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
os_linux_mipsx.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_linux_noauxv.go
…
os_linux_ppc64x.go
…
os_linux_s390x.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
os_linux.go
runtime: move startupRandomData back to runtime2.go
2021-01-01 15:11:45 -08:00
os_netbsd_arm64.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_netbsd.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
os_only_solaris.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
os_openbsd.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
os_solaris.go
runtime: correct semaphore implementation on netbsd
2020-10-14 13:56:01 -07:00
os_windows_arm.go
…
panic32.go
…
panic_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
panic.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
preempt_nonwindows.go
libgo: update to Go1.14rc1 release
2020-02-15 09:14:10 -08:00
preempt.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
print.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
proc_runtime_test.go
…
proc_test.go
libgo: update to Go 1.15.3 release
2020-10-27 13:58:02 -07:00
proc.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
profbuf_test.go
…
profbuf.go
…
proflabel.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
race0.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
rand_test.go
…
rdebug.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
relax_stub.go
…
runtime1.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
runtime2.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
runtime_mmap_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
runtime_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
runtime_unix_test.go
…
runtime-lldb_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
runtime.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
rwmutex_test.go
…
rwmutex.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
select.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
sema_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
sema.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
semasleep_test.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
signal_gccgo.go
libgo: handle linking to NetBSD's versioned symbols
2020-10-28 18:20:50 -07:00
signal_unix.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
signal_windows_test.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
sigqueue_note.go
…
sigqueue.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
sizeclasses.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
sizeof_test.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
slice_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
slice.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
stack_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
string_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
string.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
stubs2.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
stubs3.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
stubs_linux.go
…
stubs_nonlinux.go
…
stubs.go
libgo: ensure memmove, memset 8 byte atomicity on ppc64x
2021-02-25 17:01:23 -08:00
symtab_test.go
…
symtab.go
compiler, libgo: change mangling scheme
2020-11-20 12:44:35 -08:00
sys_wasm.go
…
time_fake.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
time_nofake.go
libgo: update to Go1.14beta1
2020-01-21 23:53:22 -08:00
time_test.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
time.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
timeasm.go
…
timestub2.go
libgo: update to Go1.16rc1
2021-01-29 11:04:55 -08:00
timestub.go
…
trace.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
traceback_gccgo.go
libgo: update to Go1.16beta1 release
2020-12-30 15:13:24 -08:00
type.go
libgo: update to go1.15rc1
2020-08-01 11:21:40 -07:00
typekind.go
…
utf8.go
libgo: update to Go1.14rc1 release
2020-02-15 09:14:10 -08:00
write_err_android.go
…
write_err.go
…