diff options
| author | Russ Cox <rsc@golang.org> | 2015-01-14 21:47:49 -0500 |
|---|---|---|
| committer | Russ Cox <rsc@golang.org> | 2015-01-19 15:27:23 +0000 |
| commit | 4d226dfee9d08a1e39cab5fe03b4d820b4a75d56 (patch) | |
| tree | ff55466827774a2e3b4a2ec3b140dd8f403b1060 /src/runtime/stack1.go | |
| parent | 7ef59e4ed8c2bc4d79d1a40ece6e262677214ace (diff) | |
| download | go-4d226dfee9d08a1e39cab5fe03b4d820b4a75d56.tar.xz | |
runtime: move write barrier code into mbarrier.go
I also added new comments at the top of mbarrier.go,
but the rest of the code is just copy-and-paste.
Change-Id: Iaeb2b12f8b1eaa33dbff5c2de676ca902bfddf2e
Reviewed-on: https://go-review.googlesource.com/2990
Reviewed-by: Austin Clements <austin@google.com>
Diffstat (limited to 'src/runtime/stack1.go')
| -rw-r--r-- | src/runtime/stack1.go | 3 |
1 files changed, 1 insertions, 2 deletions
diff --git a/src/runtime/stack1.go b/src/runtime/stack1.go index 743e1073c6..0f31a32e7f 100644 --- a/src/runtime/stack1.go +++ b/src/runtime/stack1.go @@ -22,7 +22,6 @@ const ( const ( uintptrMask = 1<<(8*ptrSize) - 1 - poisonGC = uintptrMask & 0xf969696969696969 poisonStack = uintptrMask & 0x6868686868686868 // Goroutine preemption request. @@ -389,7 +388,7 @@ func adjustpointers(scanp unsafe.Pointer, cbv *bitvector, adjinfo *adjustinfo, f case _BitsPointer: p := *(*unsafe.Pointer)(add(scanp, i*ptrSize)) up := uintptr(p) - if f != nil && 0 < up && up < _PageSize && debug.invalidptr != 0 || up == poisonGC || up == poisonStack { + if f != nil && 0 < up && up < _PageSize && debug.invalidptr != 0 || up == poisonStack { // Looks like a junk value in a pointer slot. // Live analysis wrong? getg().m.traceback = 2 |