Home
last modified time | relevance | path

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

12345678910>>...164

/freebsd-12.1/sys/compat/linuxkpi/common/include/linux/
H A Dio.h52 #define __raw_readb(addr) __raw_readb(addr) argument
120 #define readb(addr) readb(addr) argument
130 #define writeb(v, addr) writeb(v, addr) argument
143 #define readw(addr) readw(addr) argument
153 #define writew(v, addr) writew(v, addr) argument
166 #define readl(addr) readl(addr) argument
176 #define writel(v, addr) writel(v, addr) argument
191 #define readq(addr) readq(addr) argument
279 #define ioread8(addr) ioread8(addr) argument
287 #define ioread16(addr) ioread16(addr) argument
[all …]
H A Detherdevice.h55 is_zero_ether_addr(const u8 * addr) in is_zero_ether_addr() argument
57 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == 0x00); in is_zero_ether_addr()
61 is_multicast_ether_addr(const u8 * addr) in is_multicast_ether_addr() argument
63 return (0x01 & addr[0]); in is_multicast_ether_addr()
67 is_broadcast_ether_addr(const u8 * addr) in is_broadcast_ether_addr() argument
69 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == (6 * 0xff)); in is_broadcast_ether_addr()
73 is_valid_ether_addr(const u8 * addr) in is_valid_ether_addr() argument
75 return !is_multicast_ether_addr(addr) && !is_zero_ether_addr(addr); in is_valid_ether_addr()
/freebsd-12.1/contrib/compiler-rt/lib/tsan/rtl/
H A Dtsan_interface.cc35 void __tsan_read16(void *addr) { in __tsan_read16() argument
40 void __tsan_write16(void *addr) { in __tsan_write16() argument
94 __tsan_unaligned_read2(addr); in __sanitizer_unaligned_load16()
95 return *addr; in __sanitizer_unaligned_load16()
100 __tsan_unaligned_read4(addr); in __sanitizer_unaligned_load32()
101 return *addr; in __sanitizer_unaligned_load32()
106 __tsan_unaligned_read8(addr); in __sanitizer_unaligned_load64()
107 return *addr; in __sanitizer_unaligned_load64()
113 *addr = v; in __sanitizer_unaligned_store16()
119 *addr = v; in __sanitizer_unaligned_store32()
[all …]
H A Dtsan_interface_inl.h21 void __tsan_read1(void *addr) { in __tsan_read1() argument
25 void __tsan_read2(void *addr) { in __tsan_read2() argument
29 void __tsan_read4(void *addr) { in __tsan_read4() argument
33 void __tsan_read8(void *addr) { in __tsan_read8() argument
37 void __tsan_write1(void *addr) { in __tsan_write1() argument
41 void __tsan_write2(void *addr) { in __tsan_write2() argument
45 void __tsan_write4(void *addr) { in __tsan_write4() argument
49 void __tsan_write8(void *addr) { in __tsan_write8() argument
53 void __tsan_read1_pc(void *addr, void *pc) { in __tsan_read1_pc() argument
57 void __tsan_read2_pc(void *addr, void *pc) { in __tsan_read2_pc() argument
[all …]
H A Dtsan_interface_java.cc180 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock()
191 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_unlock()
194 MutexUnlock(thr, pc, addr); in __tsan_java_mutex_unlock()
201 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_read_lock()
212 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_read_unlock()
215 MutexReadUnlock(thr, pc, addr); in __tsan_java_mutex_read_unlock()
222 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock_rec()
234 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_unlock_rec()
244 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_acquire()
247 Acquire(thr, caller_pc, addr); in __tsan_java_acquire()
[all …]
/freebsd-12.1/contrib/gcc/
H A Dtree-ssa-address.c127 *addr = gen_rtx_PLUS (Pmode, *addr, base); in gen_addr_rtx()
144 *addr = gen_rtx_PLUS (Pmode, *addr, act_elem); in gen_addr_rtx()
152 *addr = gen_rtx_PLUS (Pmode, *addr, offset); in gen_addr_rtx()
180 if (addr->step && !integer_onep (addr->step)) in addr_for_mem_ref()
215 templ = templates + TEMPL_IDX (addr->symbol, addr->base, addr->index, in addr_for_mem_ref()
327 if (addr->offset && zero_p (addr->offset)) in create_mem_ref_raw()
331 addr->symbol, addr->base, addr->index, in create_mem_ref_raw()
332 addr->step, addr->offset, NULL, NULL); in create_mem_ref_raw()
481 addr->coefs[j] = addr->coefs[i]; in most_expensive_mult_to_index()
482 addr->elts[j] = addr->elts[i]; in most_expensive_mult_to_index()
[all …]
/freebsd-12.1/sys/ddb/
H A Ddb_examine.c115 addr += size; in db_examine()
120 addr += size; in db_examine()
125 addr += size; in db_examine()
130 addr += size; in db_examine()
135 addr += size; in db_examine()
145 addr += 1; in db_examine()
170 addr = db_disasm(addr, false); in db_examine()
173 addr = db_disasm(addr, true); in db_examine()
184 db_next = addr; in db_examine()
258 db_addr_t addr; in db_search_cmd() local
[all …]
/freebsd-12.1/sys/mips/nlm/hal/
H A Dhaldefs.h73 nlm_load_word(uint64_t addr) in nlm_load_word() argument
199 : "r"(addr)); in nlm_load_word_daddr()
212 : : "r"(val), "r"(addr) in nlm_store_word_daddr()
227 : "r"(addr)); in nlm_load_dword_daddr()
239 : : "r"(val), "r"(addr) in nlm_store_dword_daddr()
249 addrhi = addr >> 32; in nlm_load_word_daddr()
276 addrhi = addr >> 32; in nlm_store_word_daddr()
300 addrh = addr >> 32; in nlm_load_dword_daddr()
329 addrh = addr >> 32; in nlm_store_dword_daddr()
359 return *addr; in nlm_read_reg()
[all …]
/freebsd-12.1/contrib/binutils/bfd/
H A Dlibbfd.c524 return (addr[0] << 8) | addr[1]; in bfd_getb16()
531 return (addr[1] << 8) | addr[0]; in bfd_getl16()
538 return COERCE16 ((addr[0] << 8) | addr[1]); in bfd_getb_signed_16()
545 return COERCE16 ((addr[1] << 8) | addr[0]); in bfd_getl_signed_16()
551 bfd_byte *addr = p; in bfd_putb16() local
559 bfd_byte *addr = p; in bfd_putl16() local
630 v |= addr[7]; in bfd_getb64()
653 v |= addr[0]; in bfd_getl64()
677 v |= addr[7]; in bfd_getb_signed_64()
700 v |= addr[0]; in bfd_getl_signed_64()
[all …]
/freebsd-12.1/stand/i386/libi386/
H A Dsmbios.c74 caddr_t addr; member
108 for (cp = addr; cp < addr + len; cp += SMBIOS_STEP) in smbios_sigsearch()
125 cp = SMBIOS_GETSTR(addr); in smbios_getstring()
203 f1, f2, f3, SMBIOS_GET8(addr, 8), SMBIOS_GET8(addr, 9), in smbios_setuuid()
204 SMBIOS_GET8(addr, 10), SMBIOS_GET8(addr, 11), in smbios_setuuid()
205 SMBIOS_GET8(addr, 12), SMBIOS_GET8(addr, 13), in smbios_setuuid()
206 SMBIOS_GET8(addr, 14), SMBIOS_GET8(addr, 15)); in smbios_setuuid()
344 if (smbios.addr == NULL) in smbios_find_struct()
372 saddr = smbios_sigsearch(addr ? addr : PTOV(SMBIOS_START), in smbios_probe()
414 smbios_probe(addr); in smbios_detect()
[all …]
/freebsd-12.1/tests/sys/netinet/
H A Dso_reuseport_lb_test.c72 error = connect(sd, addr, addr->sa_len); in lb_simple_accept_loop()
137 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
138 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
142 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
154 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
155 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
193 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
194 addr.sin6_len = sizeof(addr); in ATF_TC_BODY()
198 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
210 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
[all …]
/freebsd-12.1/contrib/jemalloc/src/
H A Dpages.c55 assert(ALIGNMENT_ADDR2BASE(addr, os_page) == addr); in os_pages_map()
85 } else if (addr != NULL && ret != addr) { in os_pages_map()
93 assert(ret == NULL || (addr == NULL && ret != addr) || (addr != NULL && in os_pages_map()
213 assert(PAGE_ADDR2BASE(addr) == addr); in pages_unmap()
221 assert(PAGE_ADDR2BASE(addr) == addr); in pages_commit_impl()
264 assert(PAGE_ADDR2BASE(addr) == addr); in pages_purge_lazy()
299 assert(PAGE_ADDR2BASE(addr) == addr); in pages_purge_forced()
320 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_huge_impl()
343 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_nohuge_impl()
366 assert(PAGE_ADDR2BASE(addr) == addr); in pages_dontdump()
[all …]
/freebsd-12.1/sys/powerpc/powerpc/
H A Dbus_machdep.c85 earlyboot_mappings[earlyboot_map_idx].addr = addr; in bs_gen_map()
190 res = *addr; in bs_be_rs_1()
203 res = *addr; in bs_be_rs_2()
216 res = *addr; in bs_be_rs_4()
229 res = *addr; in bs_be_rs_8()
304 *addr = val; in bs_be_ws_1()
315 *addr = val; in bs_be_ws_2()
326 *addr = val; in bs_be_ws_4()
337 *addr = val; in bs_be_ws_8()
504 res = *addr; in bs_le_rs_1()
[all …]
/freebsd-12.1/contrib/compiler-rt/lib/asan/
H A Dasan_descriptions.cc99 descr->addr = addr; in GetShadowAddressInformation()
108 descr->bad_addr = addr; in GetAccessToHeapChunkInformation()
163 descr->addr = addr; in GetHeapAddressInformation()
200 descr->addr = addr; in GetStackAddressInformation()
233 if (addr >= var.beg) { in PrintAccessAndVarIntersection()
244 else if (addr >= prev_var_end && addr - prev_var_end >= var.beg - addr_end) in PrintAccessAndVarIntersection()
283 if (addr < g.beg) { in DescribeAddressRelativeToGlobal()
287 if (addr < g.beg + g.size) addr = g.beg + g.size; in DescribeAddressRelativeToGlobal()
292 str.append("%p is located %zd bytes inside", (void *)addr, addr - g.beg); in DescribeAddressRelativeToGlobal()
305 descr->addr = addr; in GetGlobalAddressInformation()
[all …]
/freebsd-12.1/sys/mips/nlm/
H A Dbus_space_rmi_pci.c441 addr++; in rmi_pci_bus_space_read_multi_1()
452 *addr = bswap16(*addr); in rmi_pci_bus_space_read_multi_2()
453 addr++; in rmi_pci_bus_space_read_multi_2()
464 *addr = bswap32(*addr); in rmi_pci_bus_space_read_multi_4()
465 addr++; in rmi_pci_bus_space_read_multi_4()
512 addr++; in rmi_pci_bus_space_write_multi_1()
523 addr++; in rmi_pci_bus_space_write_multi_2()
534 addr++; in rmi_pci_bus_space_write_multi_4()
612 addr++; in rmi_pci_bus_space_read_multi_stream_1()
622 addr++; in rmi_pci_bus_space_read_multi_stream_2()
[all …]
/freebsd-12.1/contrib/gdb/gdb/
H A Dsparc64fbsd-tdep.c128 cache->saved_regs[SPARC64_FPRS_REGNUM].addr = addr + 0 * 8; in sparc64fbsd_sigtramp_frame_cache()
129 cache->saved_regs[SPARC64_FSR_REGNUM].addr = addr + 1 * 8; in sparc64fbsd_sigtramp_frame_cache()
134 cache->saved_regs[SPARC64_NPC_REGNUM].addr = addr + 0 * 8; in sparc64fbsd_sigtramp_frame_cache()
135 cache->saved_regs[SPARC64_PC_REGNUM].addr = addr + 1 * 8; in sparc64fbsd_sigtramp_frame_cache()
137 cache->saved_regs[SPARC64_Y_REGNUM].addr = addr + 4 * 8; in sparc64fbsd_sigtramp_frame_cache()
144 cache->saved_regs[regnum].addr = addr; in sparc64fbsd_sigtramp_frame_cache()
148 addr = cache->saved_regs[SPARC_SP_REGNUM].addr; in sparc64fbsd_sigtramp_frame_cache()
152 cache->saved_regs[regnum].addr = addr; in sparc64fbsd_sigtramp_frame_cache()
159 addr = cache->saved_regs[SPARC64_FPRS_REGNUM].addr; in sparc64fbsd_sigtramp_frame_cache()
165 cache->saved_regs[regnum].addr = addr; in sparc64fbsd_sigtramp_frame_cache()
[all …]
H A Di386-nat.c258 if (addr || len) in i386_show_dr()
352 && dr_mirror[i] == addr in i386_insert_aligned_watchpoint()
374 dr_mirror[i] = addr; in i386_insert_aligned_watchpoint()
389 I386_DR_LOW_SET_ADDR (i, addr); in i386_insert_aligned_watchpoint()
409 && dr_mirror[i] == addr in i386_remove_aligned_watchpoint()
497 addr += size; in i386_handle_nonaligned_watchpoint()
514 || addr % len != 0) in i386_insert_watchpoint()
538 || addr % len != 0) in i386_remove_watchpoint()
573 CORE_ADDR addr = 0; in i386_stopped_data_address() local
588 addr = dr_mirror[i]; in i386_stopped_data_address()
[all …]
/freebsd-12.1/usr.sbin/ppp/
H A Dcbcp.c252 addr = (struct cbcp_addr *)(addr->addr + strlen(addr->addr) + 1); in cbcp_data_Show()
278 *addr->addr = '\0'; in cbcp_SendReq()
289 strncpy(addr->addr, next, sizeof addr->addr - 1); in cbcp_SendReq()
290 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendReq()
468 addr = (struct cbcp_addr *)(addr->addr + strlen(addr->addr) + 1); in cbcp_AdjustResponse()
497 strncpy(addr->addr, cbcp->fsm.phone, sizeof addr->addr - 1); in cbcp_SendResponse()
498 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendResponse()
499 data.length = (addr->addr + strlen(addr->addr) + 1) - (char *)&data; in cbcp_SendResponse()
605 strncpy(addr->addr, cbcp->fsm.phone, sizeof addr->addr - 1); in cbcp_SendAck()
606 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendAck()
[all …]
H A Diface.c180 realloc(iface->addr, (iface->addrs + 1) * sizeof iface->addr[0]); in iface_Create()
183 iface->addr = addr; in iface_Create()
515 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Clear()
571 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Add()
586 (iface->addr, (iface->addrs + 1) * sizeof iface->addr[0]); in iface_Add()
587 if (addr == NULL) { in iface_Add()
592 iface->addr = addr; in iface_Add()
605 bcopy(iface->addr, iface->addr + 1, iface->addrs * sizeof *iface->addr); in iface_Add()
610 memcpy(iface->addr + n, &newaddr, sizeof(*iface->addr)); in iface_Add()
635 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Delete()
[all …]
H A Dncpaddr.c197 switch (addr->ncpaddr_family) { in ncpaddr_isdefault()
220 switch (addr->ncpaddr_family) { in ncpaddr_equal()
259 addr->ncpaddr_family = AF_INET; in ncpaddr_setip4addr()
275 addr->ncpaddr_family = AF_INET; in ncpaddr_setip4()
276 addr->ncpaddr_ip4addr = ip; in ncpaddr_setip4()
284 *ip = addr->ncpaddr_ip4addr; in ncpaddr_getip4()
293 addr->ncpaddr_ip6addr = *ip6; in ncpaddr_setip6()
301 *ip6 = addr->ncpaddr_ip6addr; in ncpaddr_getip6()
406 return ncpaddr_ntowa(addr); in ncpaddr_ntoa()
849 struct ncpaddr addr; in ncprange_ntoa() local
[all …]
/freebsd-12.1/contrib/llvm/tools/clang/lib/Headers/
H A Davx512pfintrin.h36 (void const *)(addr), (int)(scale), \
39 #define _mm512_prefetch_i32gather_pd(index, addr, scale, hint) \ argument
41 (void const *)(addr), (int)(scale), \
49 #define _mm512_prefetch_i32gather_ps(index, addr, scale, hint) \ argument
59 #define _mm512_prefetch_i64gather_pd(index, addr, scale, hint) \ argument
68 #define _mm512_prefetch_i64gather_ps(index, addr, scale, hint) \ argument
72 #define _mm512_prefetch_i32scatter_pd(addr, index, scale, hint) \ argument
74 (void *)(addr), (int)(scale), \
79 (void *)(addr), (int)(scale), \
93 (void *)(addr), (int)(scale), \
[all …]
/freebsd-12.1/contrib/libunwind/src/
H A DAddressSpace.hpp234 return get64(addr); in getP()
236 return get32(addr); in getP()
242 return get64(addr); in getRegister()
244 return get32(addr); in getRegister()
269 addr = (pint_t) p; in getULEB128()
290 addr = (pint_t) p; in getSLEB128()
306 addr = (pint_t) p; in getEncodedP()
314 addr = (pint_t) p; in getEncodedP()
319 addr = (pint_t) p; in getEncodedP()
324 addr = (pint_t) p; in getEncodedP()
[all …]
/freebsd-12.1/sys/arm/arm/
H A Dmachdep_ptrace.c235 addr += 8; in arm_predict_branch()
277 addr = pc + 8 + (addr << 2); in arm_predict_branch()
278 error = read_int(cookie, addr, &addr); in arm_predict_branch()
279 *new_pc = addr; in arm_predict_branch()
294 error = read_int(cookie, addr, &addr); in arm_predict_branch()
295 *new_pc = addr; in arm_predict_branch()
307 addr = addr - 0; in arm_predict_branch()
310 addr = addr + 0 + ((nregs - 1) << 2); in arm_predict_branch()
313 addr = addr - 4; in arm_predict_branch()
316 addr = addr + 4 + ((nregs - 1) << 2); in arm_predict_branch()
[all …]
/freebsd-12.1/sys/vm/
H A Dvm_kern.c150 return (addr); in kva_alloc()
229 return (addr); in kmem_alloc_attr_domain()
253 if (addr != 0) in kmem_alloc_attr_domainset()
257 return (addr); in kmem_alloc_attr_domainset()
312 tmp = addr; in kmem_alloc_contig_domain()
322 return (addr); in kmem_alloc_contig_domain()
351 return (addr); in kmem_alloc_contig_domainset()
420 return (addr); in kmem_malloc_domain()
444 return (addr); in kmem_malloc_domainset()
526 for (start = addr, end = addr + size; addr < end; addr = next) { in kmem_back()
[all …]
H A Dvm_mmap.c292 if (addr + size < addr) in kern_mmap()
473 if (addr + size < addr) in kern_msync()
533 if (addr + size < addr) in kern_munmap()
614 if (addr + size < addr) in kern_mprotect()
643 addr = (vm_offset_t)uap->addr; in sys_minherit()
651 if (addr + size < addr) in sys_minherit()
704 if ((addr + len) < addr) in kern_madvise()
1010 if (last < addr || end < addr) in kern_mlock()
1180 if (last < addr || end < addr) in kern_munlock()
1499 *addr = round_page(*addr); in vm_mmap_object()
[all …]

12345678910>>...164