Home
last modified time | relevance | path

Searched refs:addr (Results 1 – 25 of 4694) sorted by relevance

12345678910>>...188

/netbsd-src/sys/external/bsd/compiler_rt/dist/lib/tsan/rtl/
H A Dtsan_interface.cc35 void __tsan_read16(void *addr) { in __tsan_read16() argument
36 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_read16()
37 MemoryRead(cur_thread(), CALLERPC, (uptr)addr + 8, kSizeLog8); in __tsan_read16()
40 void __tsan_write16(void *addr) { in __tsan_write16() argument
41 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_write16()
42 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr + 8, kSizeLog8); in __tsan_write16()
45 void __tsan_read16_pc(void *addr, void *pc) { in __tsan_read16_pc() argument
46 MemoryRead(cur_thread(), (uptr)pc, (uptr)addr, kSizeLog8); in __tsan_read16_pc()
47 MemoryRead(cur_thread(), (uptr)pc, (uptr)addr + 8, kSizeLog8); in __tsan_read16_pc()
50 void __tsan_write16_pc(void *addr, void *pc) { in __tsan_write16_pc() argument
[all …]
H A Dtsan_interface_inl.h21 void __tsan_read1(void *addr) { in __tsan_read1() argument
22 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog1); in __tsan_read1()
25 void __tsan_read2(void *addr) { in __tsan_read2() argument
26 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog2); in __tsan_read2()
29 void __tsan_read4(void *addr) { in __tsan_read4() argument
30 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog4); in __tsan_read4()
33 void __tsan_read8(void *addr) { in __tsan_read8() argument
34 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_read8()
37 void __tsan_write1(void *addr) { in __tsan_write1() argument
38 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr, kSizeLog1); in __tsan_write1()
[all …]
/netbsd-src/external/gpl3/gcc.old/dist/libsanitizer/tsan/
H A Dtsan_interface.cc35 void __tsan_read16(void *addr) { in __tsan_read16() argument
36 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_read16()
37 MemoryRead(cur_thread(), CALLERPC, (uptr)addr + 8, kSizeLog8); in __tsan_read16()
40 void __tsan_write16(void *addr) { in __tsan_write16() argument
41 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_write16()
42 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr + 8, kSizeLog8); in __tsan_write16()
45 void __tsan_read16_pc(void *addr, void *pc) { in __tsan_read16_pc() argument
46 MemoryRead(cur_thread(), (uptr)pc, (uptr)addr, kSizeLog8); in __tsan_read16_pc()
47 MemoryRead(cur_thread(), (uptr)pc, (uptr)addr + 8, kSizeLog8); in __tsan_read16_pc()
50 void __tsan_write16_pc(void *addr, void *pc) { in __tsan_write16_pc() argument
[all …]
H A Dtsan_interface_inl.h19 void __tsan_read1(void *addr) { in __tsan_read1() argument
20 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog1); in __tsan_read1()
23 void __tsan_read2(void *addr) { in __tsan_read2() argument
24 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog2); in __tsan_read2()
27 void __tsan_read4(void *addr) { in __tsan_read4() argument
28 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog4); in __tsan_read4()
31 void __tsan_read8(void *addr) { in __tsan_read8() argument
32 MemoryRead(cur_thread(), CALLERPC, (uptr)addr, kSizeLog8); in __tsan_read8()
35 void __tsan_write1(void *addr) { in __tsan_write1() argument
36 MemoryWrite(cur_thread(), CALLERPC, (uptr)addr, kSizeLog1); in __tsan_write1()
[all …]
/netbsd-src/external/gpl3/binutils.old/dist/bfd/
H A Dlibbfd.c625 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getb16() local
626 return (addr[0] << 8) | addr[1]; in bfd_getb16()
632 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getl16() local
633 return (addr[1] << 8) | addr[0]; in bfd_getl16()
639 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getb_signed_16() local
640 return COERCE16 ((addr[0] << 8) | addr[1]); in bfd_getb_signed_16()
646 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getl_signed_16() local
647 return COERCE16 ((addr[1] << 8) | addr[0]); in bfd_getl_signed_16()
653 bfd_byte *addr = (bfd_byte *) p; in bfd_putb16() local
654 addr[0] = (data >> 8) & 0xff; in bfd_putb16()
[all …]
/netbsd-src/external/gpl3/gcc/dist/libsanitizer/tsan/
H A Dtsan_interface.inc21 void __tsan_read1(void *addr) {
22 MemoryAccess(cur_thread(), CALLERPC, (uptr)addr, 1, kAccessRead);
25 void __tsan_read2(void *addr) {
26 MemoryAccess(cur_thread(), CALLERPC, (uptr)addr, 2, kAccessRead);
29 void __tsan_read4(void *addr) {
30 MemoryAccess(cur_thread(), CALLERPC, (uptr)addr, 4, kAccessRead);
33 void __tsan_read8(void *addr) {
34 MemoryAccess(cur_thread(), CALLERPC, (uptr)addr, 8, kAccessRead);
37 void __tsan_write1(void *addr) {
38 MemoryAccess(cur_thread(), CALLERPC, (uptr)addr, 1, kAccessWrite);
[all …]
H A Dtsan_interface_java.cpp40 MBlock *JavaHeapBlock(uptr addr, uptr *start) { in JavaHeapBlock() argument
41 if (!jctx || addr < jctx->heap_begin || in JavaHeapBlock()
42 addr >= jctx->heap_begin + jctx->heap_size) in JavaHeapBlock()
44 for (uptr p = RoundDown(addr, kMetaShadowCell); p >= jctx->heap_begin; in JavaHeapBlock()
49 if (p + b->siz <= addr) in JavaHeapBlock()
162 void __tsan_java_mutex_lock(jptr addr) { in __tsan_java_mutex_lock() argument
164 DPrintf("#%d: java_mutex_lock(0x%zx)\n", thr->tid, addr); in __tsan_java_mutex_lock()
166 DCHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock()
167 DCHECK_LT(addr, jctx->heap_begin + jctx->heap_size); in __tsan_java_mutex_lock()
169 MutexPostLock(thr, 0, addr, in __tsan_java_mutex_lock()
[all …]
/netbsd-src/external/gpl3/binutils/dist/bfd/
H A Dlibbfd.c743 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getb16() local
744 return (addr[0] << 8) | addr[1]; in bfd_getb16()
750 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getl16() local
751 return (addr[1] << 8) | addr[0]; in bfd_getl16()
757 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getb_signed_16() local
758 return COERCE16 ((addr[0] << 8) | addr[1]); in bfd_getb_signed_16()
764 const bfd_byte *addr = (const bfd_byte *) p; in bfd_getl_signed_16() local
765 return COERCE16 ((addr[1] << 8) | addr[0]); in bfd_getl_signed_16()
771 bfd_byte *addr = (bfd_byte *) p; in bfd_putb16() local
772 addr[0] = (data >> 8) & 0xff; in bfd_putb16()
[all …]
/netbsd-src/external/gpl3/gcc.old/dist/gcc/
H A Dtree-ssa-address.c112 rtx *addr, rtx **step_p, rtx **offset_p) in gen_addr_rtx() argument
116 *addr = NULL_RTX; in gen_addr_rtx()
133 *addr = act_elem; in gen_addr_rtx()
138 if (*addr) in gen_addr_rtx()
139 *addr = simplify_gen_binary (PLUS, address_mode, base, *addr); in gen_addr_rtx()
141 *addr = base; in gen_addr_rtx()
160 if (*addr) in gen_addr_rtx()
161 *addr = gen_rtx_PLUS (address_mode, *addr, act_elem); in gen_addr_rtx()
163 *addr = act_elem; in gen_addr_rtx()
167 if (*addr) in gen_addr_rtx()
[all …]
/netbsd-src/external/gpl3/gcc/dist/gcc/
H A Dtree-ssa-address.cc112 rtx *addr, rtx **step_p, rtx **offset_p) in gen_addr_rtx() argument
116 *addr = NULL_RTX; in gen_addr_rtx()
133 *addr = act_elem; in gen_addr_rtx()
138 if (*addr) in gen_addr_rtx()
139 *addr = simplify_gen_binary (PLUS, address_mode, base, *addr); in gen_addr_rtx()
141 *addr = base; in gen_addr_rtx()
160 if (*addr) in gen_addr_rtx()
161 *addr = gen_rtx_PLUS (address_mode, *addr, act_elem); in gen_addr_rtx()
163 *addr = act_elem; in gen_addr_rtx()
167 if (*addr) in gen_addr_rtx()
[all …]
/netbsd-src/usr.sbin/npf/npftest/libnpftest/
H A Dnpf_table_test.c66 check_ip4(const npf_addr_t *addr, const char *ipstr) in check_ip4() argument
71 return memcmp(addr, test_addr, alen) == 0; in check_ip4()
77 npf_addr_t addr_storage, *addr = &addr_storage; in ip4list_insert_lookup() local
81 addr->word32[0] = inet_addr(ip_list[i]); in ip4list_insert_lookup()
82 error = npf_table_insert(t, alen, addr, NPF_NO_NETMASK); in ip4list_insert_lookup()
84 error = npf_table_lookup(t, alen, addr); in ip4list_insert_lookup()
92 npf_addr_t addr_storage, *addr = &addr_storage; in fill_with_ip4() local
100 addr->word32[0] = inet_addr(ip_list[i]); in fill_with_ip4()
103 error = npf_table_insert(t, alen, addr, nm); in fill_with_ip4()
105 error = npf_table_insert(t, alen, addr, nm); in fill_with_ip4()
[all …]
/netbsd-src/sys/ddb/
H A Ddb_examine.c57 db_examine_cmd(db_expr_t addr, bool have_addr, db_expr_t count, in db_examine_cmd() argument
66 db_examine((db_addr_t) addr, db_examine_format, count); in db_examine_cmd()
70 db_examine(db_addr_t addr, char *fmt, int count) in db_examine() argument
87 db_printsym(addr, DB_STGY_ANY, db_printf); in db_examine()
89 db_prev = addr; in db_examine()
113 db_printf("= 0x%lx\n", (long)addr); in db_examine()
117 value = db_get_value(addr, size, false); in db_examine()
118 addr += size; in db_examine()
124 value = db_get_qvalue(addr, size, true); in db_examine()
125 addr += size; in db_examine()
[all …]
/netbsd-src/sys/arch/arm/arm32/
H A Ddb_interface.c201 db_validate_address(vaddr_t addr) in db_validate_address() argument
207 addr >= VM_MIN_KERNEL_ADDRESS in db_validate_address()
213 return pmap_extract(pmap, addr, NULL) == false; in db_validate_address()
220 db_read_bytes(vaddr_t addr, size_t size, char *data) in db_read_bytes() argument
222 char *src = (char *)addr; in db_read_bytes()
229 if (size == 4 && (addr & 3) == 0 && ((uintptr_t)data & 3) == 0) { in db_read_bytes()
234 if (size == 2 && (addr & 1) == 0 && ((uintptr_t)data & 1) == 0) { in db_read_bytes()
249 db_write_text(vaddr_t addr, size_t size, const char *data) in db_write_text() argument
252 ktext_write((void *)addr, data, size); in db_write_text()
259 db_write_bytes(vaddr_t addr, size_t size, const char *data) in db_write_bytes() argument
[all …]
/netbsd-src/external/gpl3/binutils.old/dist/gprofng/src/
H A DHeapMap.cc31 uint64_t addr; member
39 void *addr; member
52 mmaps->addr = (uint64_t) 0; in HeapMap()
73 HeapMap::allocate (uint64_t addr, long val) in allocate() argument
77 incoming->addr = addr; in allocate()
82 int ichain = (int) hash (addr); in allocate()
97 if ((next == NULL) || (next->addr < incoming->addr)) in allocate()
107 if (next->addr == incoming->addr) in allocate()
121 HeapMap::deallocate (uint64_t addr) in deallocate() argument
123 int ichain = (int) hash (addr); in deallocate()
[all …]
/netbsd-src/external/gpl3/binutils/dist/gprofng/src/
H A DHeapMap.cc31 uint64_t addr; member
39 void *addr; member
52 mmaps->addr = (uint64_t) 0; in HeapMap()
73 HeapMap::allocate (uint64_t addr, long val) in allocate() argument
77 incoming->addr = addr; in allocate()
82 int ichain = (int) hash (addr); in allocate()
97 if ((next == NULL) || (next->addr < incoming->addr)) in allocate()
107 if (next->addr == incoming->addr) in allocate()
121 HeapMap::deallocate (uint64_t addr) in deallocate() argument
123 int ichain = (int) hash (addr); in deallocate()
[all …]
/netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/subdev/i2c/
H A Dnouveau_nvkm_subdev_i2c_anx9805.c38 u8 addr; member
44 u8 addr; member
58 tmp = nvkm_rdi2cr(adap, pad->addr, 0x07) & ~0x10; in anx9805_bus_xfer()
59 nvkm_wri2cr(adap, pad->addr, 0x07, tmp | 0x10); in anx9805_bus_xfer()
60 nvkm_wri2cr(adap, pad->addr, 0x07, tmp); in anx9805_bus_xfer()
61 nvkm_wri2cr(adap, bus->addr, 0x43, 0x05); in anx9805_bus_xfer()
65 if ( (msg->flags & I2C_M_RD) && msg->addr == 0x50) { in anx9805_bus_xfer()
66 nvkm_wri2cr(adap, bus->addr, 0x40, msg->addr << 1); in anx9805_bus_xfer()
67 nvkm_wri2cr(adap, bus->addr, 0x41, seg); in anx9805_bus_xfer()
68 nvkm_wri2cr(adap, bus->addr, 0x42, off); in anx9805_bus_xfer()
[all …]
/netbsd-src/external/gpl3/gcc/dist/libsanitizer/asan/
H A Dasan_descriptions.cpp71 static bool GetShadowKind(uptr addr, ShadowKind *shadow_kind) { in GetShadowKind() argument
72 CHECK(!AddrIsInMem(addr)); in GetShadowKind()
73 if (AddrIsInShadowGap(addr)) { in GetShadowKind()
75 } else if (AddrIsInHighShadow(addr)) { in GetShadowKind()
77 } else if (AddrIsInLowShadow(addr)) { in GetShadowKind()
85 bool DescribeAddressIfShadow(uptr addr) { in DescribeAddressIfShadow() argument
87 if (!GetShadowAddressInformation(addr, &descr)) return false; in DescribeAddressIfShadow()
92 bool GetShadowAddressInformation(uptr addr, ShadowAddressDescription *descr) { in GetShadowAddressInformation() argument
93 if (AddrIsInMem(addr)) return false; in GetShadowAddressInformation()
95 if (!GetShadowKind(addr, &shadow_kind)) return false; in GetShadowAddressInformation()
[all …]
/netbsd-src/external/gpl3/gcc.old/dist/libsanitizer/asan/
H A Dasan_descriptions.cc70 static bool GetShadowKind(uptr addr, ShadowKind *shadow_kind) { in GetShadowKind() argument
71 CHECK(!AddrIsInMem(addr)); in GetShadowKind()
72 if (AddrIsInShadowGap(addr)) { in GetShadowKind()
74 } else if (AddrIsInHighShadow(addr)) { in GetShadowKind()
76 } else if (AddrIsInLowShadow(addr)) { in GetShadowKind()
85 bool DescribeAddressIfShadow(uptr addr) { in DescribeAddressIfShadow() argument
87 if (!GetShadowAddressInformation(addr, &descr)) return false; in DescribeAddressIfShadow()
92 bool GetShadowAddressInformation(uptr addr, ShadowAddressDescription *descr) { in GetShadowAddressInformation() argument
93 if (AddrIsInMem(addr)) return false; in GetShadowAddressInformation()
95 if (!GetShadowKind(addr, &shadow_kind)) return false; in GetShadowAddressInformation()
[all …]
/netbsd-src/sys/external/bsd/compiler_rt/dist/lib/asan/
H A Dasan_descriptions.cc72 static bool GetShadowKind(uptr addr, ShadowKind *shadow_kind) { in GetShadowKind() argument
73 CHECK(!AddrIsInMem(addr)); in GetShadowKind()
74 if (AddrIsInShadowGap(addr)) { in GetShadowKind()
76 } else if (AddrIsInHighShadow(addr)) { in GetShadowKind()
78 } else if (AddrIsInLowShadow(addr)) { in GetShadowKind()
87 bool DescribeAddressIfShadow(uptr addr) { in DescribeAddressIfShadow() argument
89 if (!GetShadowAddressInformation(addr, &descr)) return false; in DescribeAddressIfShadow()
94 bool GetShadowAddressInformation(uptr addr, ShadowAddressDescription *descr) { in GetShadowAddressInformation() argument
95 if (AddrIsInMem(addr)) return false; in GetShadowAddressInformation()
97 if (!GetShadowKind(addr, &shadow_kind)) return false; in GetShadowAddressInformation()
[all …]
/netbsd-src/sys/uvm/
H A Duvm_mmap.c71 range_test(const struct vm_map *map, vaddr_t addr, vsize_t size, bool ismmap) in range_test() argument
75 vaddr_t eaddr = addr + size; in range_test()
78 if (addr < vm_min_address) in range_test()
82 if (addr > eaddr) /* no wrapping! */ in range_test()
86 res = MD_MMAP_RANGE_TEST(addr, eaddr); in range_test()
96 round_and_check(const struct vm_map *map, vaddr_t *addr, vsize_t *size) in round_and_check() argument
98 const vsize_t pageoff = (vsize_t)(*addr & PAGE_MASK); in round_and_check()
100 *addr -= pageoff; in round_and_check()
105 } else if (*addr + *size < *addr) { in round_and_check()
109 return range_test(map, *addr, *size, false); in round_and_check()
[all …]
/netbsd-src/external/mpl/dhcp/dist/common/
H A Dinet.c39 struct iaddr subnet_number (addr, mask) in subnet_number() argument
40 struct iaddr addr; in subnet_number()
46 if (addr.len > sizeof(addr.iabuf))
48 if (addr.len != mask.len)
55 if (addr.len != mask.len)
58 rv.len = addr.len;
60 rv.iabuf [i] = addr.iabuf [i] & mask.iabuf [i];
143 u_int32_t host_addr (addr, mask) in host_addr() argument
144 struct iaddr addr; in host_addr()
151 if (addr.len > sizeof(addr.iabuf))
[all …]
/netbsd-src/external/apache2/llvm/dist/clang/lib/Headers/
H A Davx512pfintrin.h20 #define _mm512_mask_prefetch_i32gather_pd(index, mask, addr, scale, hint) \ argument
22 (void const *)(addr), (int)(scale), \
25 #define _mm512_prefetch_i32gather_pd(index, addr, scale, hint) \ argument
27 (void const *)(addr), (int)(scale), \
30 #define _mm512_mask_prefetch_i32gather_ps(index, mask, addr, scale, hint) \ argument
32 (__v16si)(__m512i)(index), (void const *)(addr), \
35 #define _mm512_prefetch_i32gather_ps(index, addr, scale, hint) \ argument
37 (__v16si)(__m512i)(index), (void const *)(addr), \
40 #define _mm512_mask_prefetch_i64gather_pd(index, mask, addr, scale, hint) \ argument
42 (void const *)(addr), (int)(scale), \
[all …]
/netbsd-src/sys/arch/sh3/sh3/
H A Dsh3_bus_space.c97 bus_size_t offset, uint8_t *addr, bus_size_t count) in bus_space_read_multi_1() argument
101 *addr++ = bus_space_read_1(tag, bsh, offset); in bus_space_read_multi_1()
106 bus_size_t offset, uint16_t *addr, bus_size_t count) in bus_space_read_multi_2() argument
110 *addr++ = bus_space_read_2(tag, bsh, offset); in bus_space_read_multi_2()
115 bus_size_t offset, uint32_t *addr, bus_size_t count) in bus_space_read_multi_4() argument
119 *addr++ = bus_space_read_4(tag, bsh, offset); in bus_space_read_multi_4()
124 bus_size_t offset, uint16_t *addr, bus_size_t count) in bus_space_read_multi_stream_2() argument
128 *addr++ = *(volatile uint16_t *)(bsh + offset); in bus_space_read_multi_stream_2()
133 bus_size_t offset, uint32_t *addr, bus_size_t count) in bus_space_read_multi_stream_4() argument
137 *addr++ = *(volatile uint32_t *)(bsh + offset); in bus_space_read_multi_stream_4()
[all …]
/netbsd-src/external/gpl3/binutils.old/dist/opcodes/
H A Dpj-dis.c45 print_insn_pj (bfd_vma addr, struct disassemble_info *info) in print_insn_pj() argument
52 if ((status = info->read_memory_func (addr, &opcode, 1, info))) in print_insn_pj()
59 if ((status = info->read_memory_func (addr + 1, &byte_2, 1, info))) in print_insn_pj()
67 int insn_start = addr; in print_insn_pj()
71 addr++; in print_insn_pj()
83 addr = (addr + 3) & ~3; in print_insn_pj()
84 if ((status = get_int (addr, &val, info))) in print_insn_pj()
89 addr += 4; in print_insn_pj()
91 if ((status = get_int (addr, &lowval, info))) in print_insn_pj()
93 addr += 4; in print_insn_pj()
[all …]
/netbsd-src/external/gpl3/binutils/dist/opcodes/
H A Dpj-dis.c45 print_insn_pj (bfd_vma addr, struct disassemble_info *info) in print_insn_pj() argument
52 if ((status = info->read_memory_func (addr, &opcode, 1, info))) in print_insn_pj()
59 if ((status = info->read_memory_func (addr + 1, &byte_2, 1, info))) in print_insn_pj()
67 int insn_start = addr; in print_insn_pj()
71 addr++; in print_insn_pj()
83 addr = (addr + 3) & ~3; in print_insn_pj()
84 if ((status = get_int (addr, &val, info))) in print_insn_pj()
89 addr += 4; in print_insn_pj()
91 if ((status = get_int (addr, &lowval, info))) in print_insn_pj()
93 addr += 4; in print_insn_pj()
[all …]

12345678910>>...188