Home
last modified time | relevance | path

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

12345678910>>...158

/freebsd-13.1/sys/compat/linuxkpi/common/include/linux/
H A Dio.h146 #define readb(addr) readb(addr) argument
156 #define writeb(v, addr) writeb(v, addr) argument
169 #define readw(addr) readw(addr) argument
179 #define writew(v, addr) writew(v, addr) argument
192 #define readl(addr) readl(addr) argument
202 #define writel(v, addr) writel(v, addr) argument
217 #define readq(addr) readq(addr) argument
226 #define writeq(v, addr) writeq(v, addr) argument
305 #define ioread8(addr) ioread8(addr) argument
313 #define ioread16(addr) ioread16(addr) argument
[all …]
H A Detherdevice.h56 is_zero_ether_addr(const u8 * addr) in is_zero_ether_addr() argument
58 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == 0x00); in is_zero_ether_addr()
62 is_multicast_ether_addr(const u8 * addr) in is_multicast_ether_addr() argument
64 return (0x01 & addr[0]); in is_multicast_ether_addr()
68 is_broadcast_ether_addr(const u8 * addr) in is_broadcast_ether_addr() argument
70 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == (6 * 0xff)); in is_broadcast_ether_addr()
74 is_valid_ether_addr(const u8 * addr) in is_valid_ether_addr() argument
76 return !is_multicast_ether_addr(addr) && !is_zero_ether_addr(addr); in is_valid_ether_addr()
/freebsd-13.1/contrib/llvm-project/compiler-rt/lib/tsan/rtl/
H A Dtsan_interface.cpp32 void __tsan_read16(void *addr) { in __tsan_read16() argument
37 void __tsan_write16(void *addr) { in __tsan_write16() argument
91 __tsan_unaligned_read2(addr); in __sanitizer_unaligned_load16()
92 return *addr; in __sanitizer_unaligned_load16()
97 __tsan_unaligned_read4(addr); in __sanitizer_unaligned_load32()
98 return *addr; in __sanitizer_unaligned_load32()
103 __tsan_unaligned_read8(addr); in __sanitizer_unaligned_load64()
104 return *addr; in __sanitizer_unaligned_load64()
110 *addr = v; in __sanitizer_unaligned_store16()
116 *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.cpp178 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock()
189 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_unlock()
192 MutexUnlock(thr, pc, addr); in __tsan_java_mutex_unlock()
199 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_read_lock()
210 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_read_unlock()
213 MutexReadUnlock(thr, pc, addr); in __tsan_java_mutex_read_unlock()
220 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock_rec()
232 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_unlock_rec()
242 CHECK_GE(addr, jctx->heap_begin); in __tsan_java_acquire()
245 Acquire(thr, caller_pc, addr); in __tsan_java_acquire()
[all …]
/freebsd-13.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-13.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-13.1/stand/libsa/
H A Dsmbios.c67 caddr_t addr; member
101 for (cp = addr; cp < addr + len; cp += SMBIOS_STEP) in smbios_sigsearch()
118 cp = SMBIOS_GETSTR(addr); in smbios_getstring()
196 f1, f2, f3, SMBIOS_GET8(addr, 8), SMBIOS_GET8(addr, 9), in smbios_setuuid()
197 SMBIOS_GET8(addr, 10), SMBIOS_GET8(addr, 11), in smbios_setuuid()
198 SMBIOS_GET8(addr, 12), SMBIOS_GET8(addr, 13), in smbios_setuuid()
199 SMBIOS_GET8(addr, 14), SMBIOS_GET8(addr, 15)); in smbios_setuuid()
422 if (smbios.addr == NULL) in smbios_find_struct()
450 saddr = smbios_sigsearch(addr ? addr : PTOV(SMBIOS_START), in smbios_probe()
492 smbios_probe(addr); in smbios_detect()
[all …]
/freebsd-13.1/tests/sys/netinet/
H A Dso_reuseport_lb_test.c73 error = connect(sd, addr, addr->sa_len); in lb_simple_accept_loop()
142 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
143 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
147 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
159 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
160 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
198 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
199 addr.sin6_len = sizeof(addr); in ATF_TC_BODY()
203 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
215 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
[all …]
/freebsd-13.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()
129 assert(ALIGNMENT_ADDR2BASE(addr, os_page) == addr); in os_pages_unmap()
242 assert(PAGE_ADDR2BASE(addr) == addr); in pages_unmap()
250 assert(PAGE_ADDR2BASE(addr) == addr); in pages_commit_impl()
328 assert(PAGE_ADDR2BASE(addr) == addr); in pages_purge_forced()
349 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_huge_impl()
372 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_nohuge_impl()
395 assert(PAGE_ADDR2BASE(addr) == addr); in pages_dontdump()
[all …]
/freebsd-13.1/contrib/llvm-project/compiler-rt/lib/asan/
H A Dasan_descriptions.cpp97 descr->addr = addr; in GetShadowAddressInformation()
106 descr->bad_addr = addr; in GetAccessToHeapChunkInformation()
161 descr->addr = addr; in GetHeapAddressInformation()
198 descr->addr = addr; in GetStackAddressInformation()
231 if (addr >= var.beg) { in PrintAccessAndVarIntersection()
242 else if (addr >= prev_var_end && addr - prev_var_end >= var.beg - addr_end) in PrintAccessAndVarIntersection()
281 if (addr < g.beg) { in DescribeAddressRelativeToGlobal()
285 if (addr < g.beg + g.size) addr = g.beg + g.size; in DescribeAddressRelativeToGlobal()
290 str.append("%p is located %zd bytes inside", (void *)addr, addr - g.beg); in DescribeAddressRelativeToGlobal()
303 descr->addr = addr; in GetGlobalAddressInformation()
[all …]
/freebsd-13.1/contrib/llvm-project/clang/lib/Headers/
H A Davx512pfintrin.h22 (void const *)(addr), (int)(scale), \
25 #define _mm512_prefetch_i32gather_pd(index, addr, scale, hint) \ argument
27 (void const *)(addr), (int)(scale), \
35 #define _mm512_prefetch_i32gather_ps(index, addr, scale, hint) \ argument
45 #define _mm512_prefetch_i64gather_pd(index, addr, scale, hint) \ argument
54 #define _mm512_prefetch_i64gather_ps(index, addr, scale, hint) \ argument
58 #define _mm512_prefetch_i32scatter_pd(addr, index, scale, hint) \ argument
60 (void *)(addr), (int)(scale), \
65 (void *)(addr), (int)(scale), \
79 (void *)(addr), (int)(scale), \
[all …]
/freebsd-13.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()
510 addr++; in rmi_pci_bus_space_write_multi_1()
521 addr++; in rmi_pci_bus_space_write_multi_2()
532 addr++; in rmi_pci_bus_space_write_multi_4()
606 addr++; in rmi_pci_bus_space_read_multi_stream_1()
616 addr++; in rmi_pci_bus_space_read_multi_stream_2()
[all …]
/freebsd-13.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 …]
/freebsd-13.1/sys/powerpc/powerpc/
H A Dbus_machdep.c85 earlyboot_mappings[earlyboot_map_idx].addr = addr; in bs_gen_map()
190 res = *addr; in native_bs_rs_1()
203 res = *addr; in native_bs_rs_2()
216 res = *addr; in native_bs_rs_4()
229 res = *addr; in native_bs_rs_8()
304 *addr = val; in native_bs_ws_1()
315 *addr = val; in native_bs_ws_2()
326 *addr = val; in native_bs_ws_4()
337 *addr = val; in native_bs_ws_8()
504 res = *addr; in swapped_bs_rs_1()
[all …]
/freebsd-13.1/sys/arm/arm/
H A Dmachdep_ptrace.c235 addr += 8; in arm_predict_branch()
274 addr = pc + 8 + (addr << 2); in arm_predict_branch()
275 error = read_int(cookie, addr, &addr); in arm_predict_branch()
276 *new_pc = addr; in arm_predict_branch()
291 error = read_int(cookie, addr, &addr); in arm_predict_branch()
292 *new_pc = addr; in arm_predict_branch()
304 addr = addr - 0; in arm_predict_branch()
307 addr = addr + 0 + ((nregs - 1) << 2); in arm_predict_branch()
310 addr = addr - 4; in arm_predict_branch()
313 addr = addr + 4 + ((nregs - 1) << 2); in arm_predict_branch()
[all …]
/freebsd-13.1/contrib/capsicum-test/
H A Dsocket.cc148 memset(&addr, 0, sizeof(addr)); in TEST()
184 memset(&addr, 0, sizeof(addr)); in TEST()
200 len = sizeof(addr); in TEST()
207 len = sizeof(addr); in TEST()
208 memset(&addr, 0, sizeof(addr)); in TEST()
220 len = sizeof(addr); in TEST()
221 memset(&addr, 0, sizeof(addr)); in TEST()
266 memset(&addr, 0, sizeof(addr)); in TEST()
279 len = sizeof(addr); in TEST()
287 memset(&addr, 0, sizeof(addr)); in TEST()
[all …]
/freebsd-13.1/contrib/sendmail/contrib/
H A Ddoublebounce.pl49 my($addr);
52 ($addr) = $hdr =~ m/<(.*)>/;
53 $addr =~ s/.*\@//;
54 return $addr;
56 if ($addr =~ /\s*\(/) {
58 $addr =~ s/.*\@//;
59 return $addr;
62 $addr =~ s/.*\@//;
63 return $addr;
74 my($addr, $from) = @_;
[all …]
/freebsd-13.1/contrib/llvm-project/compiler-rt/lib/tsan/go/
H A Dtsan_go.cpp62 cbctx.pc = addr; in SymbolizeCode()
75 addr = cbctx.pc; in SymbolizeCode()
85 uptr addr; member
98 cbctx.addr = addr; in SymbolizeData()
169 MapShadow(addr, size); in __tsan_map_shadow()
244 Acquire(thr, 0, (uptr)addr); in __tsan_acquire()
256 Release(thr, 0, (uptr)addr); in __tsan_release_merge()
265 MutexPreLock(thr, 0, addr); in __tsan_mutex_before_lock()
272 MutexPostLock(thr, 0, addr); in __tsan_mutex_after_lock()
279 MutexUnlock(thr, 0, addr); in __tsan_mutex_before_unlock()
[all …]
/freebsd-13.1/stand/common/
H A Dmetadata.c82 addr++; in md_copyenv()
88 addr++; in md_copyenv()
91 addr++; in md_copyenv()
92 return(addr); in md_copyenv()
253 addr = 0; in md_load_dual()
259 addr = roundup(addr, PAGE_SIZE); in md_load_dual()
262 envp = addr; in md_load_dual()
263 addr = md_copyenv(addr); in md_load_dual()
266 addr = roundup(addr, PAGE_SIZE); in md_load_dual()
276 fdtp = addr; in md_load_dual()
[all …]
/freebsd-13.1/usr.sbin/acpi/acpidump/
H A Dacpi_user.c136 u_long addr, end; in acpi_scan_rsd_ptr() local
146 pread(acpi_mem_fd, &addr, sizeof(uint16_t), addr); in acpi_scan_rsd_ptr()
147 addr <<= 4; in acpi_scan_rsd_ptr()
149 for (; addr < end; addr += 16) in acpi_scan_rsd_ptr()
154 for (; addr < end; addr += 16) in acpi_scan_rsd_ptr()
169 u_long addr; in acpi_find_rsd_ptr() local
174 addr = 0; in acpi_find_rsd_ptr()
179 if (addr == 0) { in acpi_find_rsd_ptr()
180 len = sizeof(addr); in acpi_find_rsd_ptr()
182 addr = 0; in acpi_find_rsd_ptr()
[all …]
/freebsd-13.1/usr.bin/sdiotool/
H A Dlinux_sdio_compat.c63 return sdio_read_1(func->dev, func->num, addr, err_ret); in sdio_readb()
67 return sdio_readb(func, addr, err_ret); in sdio_f0_readb()
79 unsigned int addr, int *err_ret) { in sdio_writeb() argument
80 *err_ret = sdio_write_1(func->dev, func->num, addr, b); in sdio_writeb()
86 unsigned int addr, int *err_ret) in sdio_f0_writeb() argument
88 if (addr < 0xF0 || addr > 0xFF) { in sdio_f0_writeb()
93 sdio_writeb(func, b, addr, err_ret); in sdio_f0_writeb()
97 unsigned int addr, int *err_ret) { in sdio_writew() argument
98 *err_ret = sdio_write_2(func->dev, func->num, addr, b); in sdio_writew()
102 unsigned int addr, int *err_ret) { in sdio_writel() argument
[all …]
/freebsd-13.1/contrib/llvm-project/compiler-rt/include/sanitizer/
H A Dasan_interface.h59 #define ASAN_POISON_MEMORY_REGION(addr, size) \ argument
60 __asan_poison_memory_region((addr), (size))
69 #define ASAN_UNPOISON_MEMORY_REGION(addr, size) \ argument
70 __asan_unpoison_memory_region((addr), (size))
72 #define ASAN_POISON_MEMORY_REGION(addr, size) \ argument
73 ((void)(addr), (void)(size))
74 #define ASAN_UNPOISON_MEMORY_REGION(addr, size) \ argument
75 ((void)(addr), (void)(size))
88 int __asan_address_is_poisoned(void const volatile *addr);
105 void __asan_describe_address(void *addr);
[all …]
/freebsd-13.1/sys/vm/
H A Dvm_kern.c154 return (addr); in kva_alloc()
257 return (addr); in kmem_alloc_attr_domain()
281 if (addr != 0) in kmem_alloc_attr_domainset()
285 return (addr); in kmem_alloc_attr_domainset()
329 tmp = addr; in kmem_alloc_contig_domain()
340 return (addr); in kmem_alloc_contig_domain()
369 return (addr); in kmem_alloc_contig_domainset()
432 return (addr); in kmem_malloc_domain()
456 return (addr); in kmem_malloc_domainset()
536 for (start = addr, end = addr + size; addr < end; addr = next) { in kmem_back()
[all …]

12345678910>>...158