/freebsd/sys/compat/linuxkpi/common/include/linux/ |
H A D | io.h | 148 #define readb(addr) readb(addr) argument 158 #define writeb(v, addr) writeb(v, addr) argument 171 #define readw(addr) readw(addr) argument 181 #define writew(v, addr) writew(v, addr) argument 194 #define readl(addr) readl(addr) argument 204 #define writel(v, addr) writel(v, addr) argument 219 #define readq(addr) readq(addr) argument 307 #define ioread8(addr) ioread8(addr) argument 315 #define ioread16(addr) ioread16(addr) argument 337 #define ioread32(addr) ioread32(addr) argument [all …]
|
H A D | etherdevice.h | 54 is_zero_ether_addr(const u8 * addr) in is_zero_ether_addr() argument 56 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == 0x00); in is_zero_ether_addr() 60 is_multicast_ether_addr(const u8 * addr) in is_multicast_ether_addr() argument 62 return (0x01 & addr[0]); in is_multicast_ether_addr() 66 is_broadcast_ether_addr(const u8 * addr) in is_broadcast_ether_addr() argument 68 return ((addr[0] + addr[1] + addr[2] + addr[3] + addr[4] + addr[5]) == (6 * 0xff)); in is_broadcast_ether_addr() 72 is_valid_ether_addr(const u8 * addr) in is_valid_ether_addr() argument 74 return !is_multicast_ether_addr(addr) && !is_zero_ether_addr(addr); in is_valid_ether_addr()
|
/freebsd/contrib/llvm-project/compiler-rt/lib/asan_abi/ |
H A D | asan_abi_shim.cpp | 72 void __asan_report_load1(uptr addr) { in __asan_report_load1() argument 186 void __asan_load1(uptr addr) { __asan_abi_load_n((void *)addr, 1, true); } in __asan_load1() argument 187 void __asan_load2(uptr addr) { __asan_abi_load_n((void *)addr, 2, true); } in __asan_load2() argument 188 void __asan_load4(uptr addr) { __asan_abi_load_n((void *)addr, 4, true); } in __asan_load4() argument 189 void __asan_load8(uptr addr) { __asan_abi_load_n((void *)addr, 8, true); } in __asan_load8() argument 190 void __asan_load16(uptr addr) { __asan_abi_load_n((void *)addr, 16, true); } in __asan_load16() argument 194 void __asan_store1(uptr addr) { __asan_abi_store_n((void *)addr, 1, true); } in __asan_store1() argument 195 void __asan_store2(uptr addr) { __asan_abi_store_n((void *)addr, 2, true); } in __asan_store2() argument 196 void __asan_store4(uptr addr) { __asan_abi_store_n((void *)addr, 4, true); } in __asan_store4() argument 197 void __asan_store8(uptr addr) { __asan_abi_store_n((void *)addr, 8, true); } in __asan_store8() argument [all …]
|
/freebsd/contrib/llvm-project/compiler-rt/lib/tsan/rtl/ |
H A D | tsan_interface.inc | 21 void __tsan_read1(void *addr) { 25 void __tsan_read2(void *addr) { 29 void __tsan_read4(void *addr) { 33 void __tsan_read8(void *addr) { 37 void __tsan_read16(void *addr) { 122 return *addr; 128 return *addr; 134 return *addr; 139 *addr = v; 145 *addr = v; [all …]
|
H A D | tsan_interface_java.cpp | 49 if (p + b->siz <= addr) in JavaHeapBlock() 166 DCHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_lock() 169 MutexPostLock(thr, 0, addr, in __tsan_java_mutex_lock() 178 DCHECK_GE(addr, jctx->heap_begin); in __tsan_java_mutex_unlock() 181 MutexUnlock(thr, 0, addr); in __tsan_java_mutex_unlock() 191 MutexPostReadLock(thr, 0, addr, in __tsan_java_mutex_read_lock() 203 MutexReadUnlock(thr, 0, addr); in __tsan_java_mutex_read_unlock() 214 MutexPostLock(thr, 0, addr, in __tsan_java_mutex_lock_rec() 237 Acquire(thr, 0, addr); in __tsan_java_acquire() 247 Release(thr, 0, addr); in __tsan_java_release() [all …]
|
H A D | tsan_rtl_mutex.cpp | 47 s->dd.ctx = s->addr; in DDMutexInit() 64 rep.AddLocation(addr, 1); in ReportMutexMisuse() 82 TraceMutexUnlock(thr, addr); in RecordMutexUnlock() 83 thr->mset.DelAddr(addr); in RecordMutexUnlock() 130 if (pc && IsAppMem(addr)) in MutexDestroy() 165 if (pc && IsAppMem(addr)) in MutexPostLock() 218 if (pc && IsAppMem(addr)) in MutexUnlock() 283 if (pc && IsAppMem(addr)) in MutexPostReadLock() 326 if (pc && IsAppMem(addr)) in MutexReadUnlock() 367 if (pc && IsAppMem(addr)) in MutexReadOrWriteUnlock() [all …]
|
/freebsd/sys/ddb/ |
H A D | db_examine.c | 112 addr += size; in db_examine() 117 addr += size; in db_examine() 122 addr += size; in db_examine() 127 addr += size; in db_examine() 132 addr += size; in db_examine() 142 addr += 1; in db_examine() 167 addr = db_disasm(addr, false); in db_examine() 170 addr = db_disasm(addr, true); in db_examine() 181 db_next = addr; in db_examine() 255 db_addr_t addr; in db_search_cmd() local [all …]
|
H A D | db_break.c | 136 bkpt->address = addr; in db_set_breakpoint() 149 db_addr_t addr) in db_delete_breakpoint() argument 158 (bkpt->address == addr)) { in db_delete_breakpoint() 173 db_addr_t addr) in db_find_breakpoint() argument 182 (bkpt->address == addr)) in db_find_breakpoint() 193 bkpt = db_find_breakpoint(&db_breakpoint, db_map_addr(addr), addr); in db_find_breakpoint_here() 197 addr); in db_find_breakpoint_here() 289 (db_addr_t)addr); in db_delete_cmd() 302 db_set_breakpoint(&db_breakpoint, db_map_addr(addr), (db_addr_t)addr, in db_breakpoint_cmd() 323 (db_addr_t)addr); in db_deletehbreak_cmd() [all …]
|
/freebsd/tests/sys/netinet/ |
H A D | so_reuseport_lb_test.c | 70 error = connect(sd, addr, addr->sa_len); in lb_simple_accept_loop() 139 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY() 140 addr.sin_len = sizeof(addr); in ATF_TC_BODY() 144 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY() 156 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY() 157 addr.sin_len = sizeof(addr); in ATF_TC_BODY() 195 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY() 196 addr.sin6_len = sizeof(addr); in ATF_TC_BODY() 200 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY() 212 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY() [all …]
|
/freebsd/contrib/jemalloc/src/ |
H A D | pages.c | 57 assert(ALIGNMENT_ADDR2BASE(addr, os_page) == addr); in os_pages_map() 87 } else if (addr != NULL && ret != addr) { in os_pages_map() 95 assert(ret == NULL || (addr == NULL && ret != addr) || (addr != NULL && in os_pages_map() 131 assert(ALIGNMENT_ADDR2BASE(addr, os_page) == addr); in os_pages_unmap() 244 assert(PAGE_ADDR2BASE(addr) == addr); in pages_unmap() 252 assert(PAGE_ADDR2BASE(addr) == addr); in pages_commit_impl() 330 assert(PAGE_ADDR2BASE(addr) == addr); in pages_purge_forced() 351 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_huge_impl() 374 assert(HUGEPAGE_ADDR2BASE(addr) == addr); in pages_nohuge_impl() 397 assert(PAGE_ADDR2BASE(addr) == addr); in pages_dontdump() [all …]
|
/freebsd/stand/libsa/ |
H A D | smbios.c | 143 caddr_t addr; member 180 for (cp = addr; cp < addr + len; cp += SMBIOS_STEP) { in smbios_sigsearch() 208 cp = SMBIOS_GETSTR(addr); in smbios_getstring() 286 f1, f2, f3, SMBIOS_GET8(addr, 8), SMBIOS_GET8(addr, 9), in smbios_setuuid() 287 SMBIOS_GET8(addr, 10), SMBIOS_GET8(addr, 11), in smbios_setuuid() 288 SMBIOS_GET8(addr, 12), SMBIOS_GET8(addr, 13), in smbios_setuuid() 289 SMBIOS_GET8(addr, 14), SMBIOS_GET8(addr, 15)); in smbios_setuuid() 522 if (smbios.addr == NULL) in smbios_find_struct() 555 saddr = smbios_sigsearch(addr ? addr : PTOV(SMBIOS_START), in smbios_probe() 612 smbios_probe(addr); in smbios_detect() [all …]
|
/freebsd/contrib/llvm-project/clang/lib/Headers/ |
H A D | avx512pfintrin.h | 19 (void const *)(addr), (int)(scale), \ 22 #define _mm512_prefetch_i32gather_pd(index, addr, scale, hint) \ argument 24 (void const *)(addr), (int)(scale), \ 32 #define _mm512_prefetch_i32gather_ps(index, addr, scale, hint) \ argument 39 (void const *)(addr), (int)(scale), \ 42 #define _mm512_prefetch_i64gather_pd(index, addr, scale, hint) \ argument 51 #define _mm512_prefetch_i64gather_ps(index, addr, scale, hint) \ argument 57 (void *)(addr), (int)(scale), \ 62 (void *)(addr), (int)(scale), \ 76 (void *)(addr), (int)(scale), \ [all …]
|
/freebsd/contrib/llvm-project/compiler-rt/lib/asan/ |
H A D | asan_descriptions.cpp | 97 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() 282 str.AppendF("%p is located %zd bytes before", (void *)addr, g.beg - addr); in DescribeAddressRelativeToGlobal() 284 if (addr < g.beg + g.size) addr = g.beg + g.size; in DescribeAddressRelativeToGlobal() 303 descr->addr = addr; in GetGlobalAddressInformation() [all …]
|
/freebsd/usr.sbin/ppp/ |
H A D | cbcp.c | 250 addr = (struct cbcp_addr *)(addr->addr + strlen(addr->addr) + 1); in cbcp_data_Show() 276 *addr->addr = '\0'; in cbcp_SendReq() 287 strncpy(addr->addr, next, sizeof addr->addr - 1); in cbcp_SendReq() 288 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendReq() 466 addr = (struct cbcp_addr *)(addr->addr + strlen(addr->addr) + 1); in cbcp_AdjustResponse() 495 strncpy(addr->addr, cbcp->fsm.phone, sizeof addr->addr - 1); in cbcp_SendResponse() 496 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendResponse() 497 data.length = (addr->addr + strlen(addr->addr) + 1) - (char *)&data; in cbcp_SendResponse() 603 strncpy(addr->addr, cbcp->fsm.phone, sizeof addr->addr - 1); in cbcp_SendAck() 604 addr->addr[sizeof addr->addr - 1] = '\0'; in cbcp_SendAck() [all …]
|
H A D | iface.c | 178 realloc(iface->addr, (iface->addrs + 1) * sizeof iface->addr[0]); in iface_Create() 181 iface->addr = addr; in iface_Create() 513 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Clear() 569 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Add() 584 (iface->addr, (iface->addrs + 1) * sizeof iface->addr[0]); in iface_Add() 585 if (addr == NULL) { in iface_Add() 590 iface->addr = addr; in iface_Add() 603 bcopy(iface->addr, iface->addr + 1, iface->addrs * sizeof *iface->addr); in iface_Add() 608 memcpy(iface->addr + n, &newaddr, sizeof(*iface->addr)); in iface_Add() 633 bcopy(iface->addr + n + 1, iface->addr + n, in iface_Delete() [all …]
|
/freebsd/sys/contrib/dev/rtw88/ |
H A D | hci.h | 121 val = rtw_read8(rtwdev, addr); in rtw_write8_set() 129 val = rtw_read16(rtwdev, addr); in rtw_write16_set() 137 val = rtw_read32(rtwdev, addr); in rtw_write32_set() 145 val = rtw_read8(rtwdev, addr); in rtw_write8_clr() 153 val = rtw_read16(rtwdev, addr); in rtw_write16_clr() 161 val = rtw_read32(rtwdev, addr); in rtw_write32_clr() 167 u32 addr, u32 mask) in rtw_read_rf() argument 220 orig = rtw_read8(rtwdev, addr); in rtw_read8_mask() 233 WARN(addr & 0x3, "should be 4-byte aligned, addr = 0x%08x\n", addr); in rtw_write32_mask() 237 rtw_write32(rtwdev, addr, set); in rtw_write32_mask() [all …]
|
/freebsd/sys/powerpc/powerpc/ |
H A D | bus_machdep.c | 83 earlyboot_mappings[earlyboot_map_idx].addr = addr; in bs_gen_map() 193 res = *addr; in native_bs_rs_1() 206 res = *addr; in native_bs_rs_2() 219 res = *addr; in native_bs_rs_4() 232 res = *addr; in native_bs_rs_8() 307 *addr = val; in native_bs_ws_1() 318 *addr = val; in native_bs_ws_2() 329 *addr = val; in native_bs_ws_4() 340 *addr = val; in native_bs_ws_8() 507 res = *addr; in swapped_bs_rs_1() [all …]
|
/freebsd/sys/arm/arm/ |
H A D | machdep_ptrace.c | 232 addr += 8; in arm_predict_branch() 271 addr = pc + 8 + (addr << 2); in arm_predict_branch() 272 error = read_int(cookie, addr, &addr); in arm_predict_branch() 273 *new_pc = addr; in arm_predict_branch() 288 error = read_int(cookie, addr, &addr); in arm_predict_branch() 289 *new_pc = addr; in arm_predict_branch() 301 addr = addr - 0; in arm_predict_branch() 304 addr = addr + 0 + ((nregs - 1) << 2); in arm_predict_branch() 307 addr = addr - 4; in arm_predict_branch() 310 addr = addr + 4 + ((nregs - 1) << 2); in arm_predict_branch() [all …]
|
/freebsd/contrib/capsicum-test/ |
H A D | socket.cc | 148 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/contrib/sendmail/contrib/ |
H A D | doublebounce.pl | 49 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/contrib/llvm-project/compiler-rt/lib/tsan/go/ |
H A D | tsan_go.cpp | 58 cbctx.pc = addr; in SymbolizeCode() 71 addr = cbctx.pc; in SymbolizeCode() 81 uptr addr; member 94 cbctx.addr = addr; in SymbolizeData() 166 MapShadow(addr, size); in __tsan_map_shadow() 241 Acquire(thr, 0, (uptr)addr); in __tsan_acquire() 253 Release(thr, 0, (uptr)addr); in __tsan_release_merge() 260 MutexPreLock(thr, 0, addr); in __tsan_mutex_before_lock() 267 MutexPostLock(thr, 0, addr); in __tsan_mutex_after_lock() 274 MutexUnlock(thr, 0, addr); in __tsan_mutex_before_unlock() [all …]
|
/freebsd/usr.sbin/acpi/acpidump/ |
H A D | acpi_user.c | 134 u_long addr, end; in acpi_scan_rsd_ptr() local 144 pread(acpi_mem_fd, &addr, sizeof(uint16_t), addr); in acpi_scan_rsd_ptr() 145 addr <<= 4; in acpi_scan_rsd_ptr() 147 for (; addr < end; addr += 16) in acpi_scan_rsd_ptr() 152 for (; addr < end; addr += 16) in acpi_scan_rsd_ptr() 167 u_long addr; in acpi_find_rsd_ptr() local 172 addr = 0; in acpi_find_rsd_ptr() 177 if (addr == 0) { in acpi_find_rsd_ptr() 178 len = sizeof(addr); in acpi_find_rsd_ptr() 180 addr = 0; in acpi_find_rsd_ptr() [all …]
|
/freebsd/sys/vm/ |
H A D | vm_kern.c | 155 return (addr); in kva_alloc() 176 return (addr); in kva_alloc_aligned() 310 void *addr; in kmem_alloc_attr_domainset() local 330 return (addr); in kmem_alloc_attr_domainset() 374 tmp = addr; in kmem_alloc_contig_domain() 404 void *addr; in kmem_alloc_contig_domainset() local 424 return (addr); in kmem_alloc_contig_domainset() 505 void *addr; in kmem_malloc_domainset() local 515 return (addr); in kmem_malloc_domainset() 595 for (start = addr, end = addr + size; addr < end; addr = next) { in kmem_back() [all …]
|
/freebsd/usr.bin/sdiotool/ |
H A D | cam_sdio.c | 34 uint32_t addr, in sdio_rw_direct() argument 91 uint32_t addr, in sdio_rw_extended() argument 328 uint32_t addr; in sdio_func_read_cis() local 337 addr = cis_addr; in sdio_func_read_cis() 353 addr += 2; in sdio_func_read_cis() 391 addr++; in sdio_func_read_cis() 411 uint32_t addr; in sdio_get_common_cis_addr() local 418 if (addr < SD_IO_CIS_START || addr > SD_IO_CIS_START + SD_IO_CIS_SIZE) { in sdio_get_common_cis_addr() 419 warn("Bad CIS address: %04X\n", addr); in sdio_get_common_cis_addr() 420 addr = 0; in sdio_get_common_cis_addr() [all …]
|
H A D | linux_sdio_compat.c | 59 return sdio_read_1(func->dev, func->num, addr, err_ret); in sdio_readb() 63 return sdio_readb(func, addr, err_ret); in sdio_f0_readb() 75 unsigned int addr, int *err_ret) { in sdio_writeb() argument 76 *err_ret = sdio_write_1(func->dev, func->num, addr, b); in sdio_writeb() 82 unsigned int addr, int *err_ret) in sdio_f0_writeb() argument 84 if (addr < 0xF0 || addr > 0xFF) { in sdio_f0_writeb() 89 sdio_writeb(func, b, addr, err_ret); in sdio_f0_writeb() 93 unsigned int addr, int *err_ret) { in sdio_writew() argument 94 *err_ret = sdio_write_2(func->dev, func->num, addr, b); in sdio_writew() 98 unsigned int addr, int *err_ret) { in sdio_writel() argument [all …]
|