Home
last modified time | relevance | path

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

12345678910>>...171

/freebsd-14.2/sys/compat/linuxkpi/common/include/linux/
H A Dio.h148 #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 Detherdevice.h54 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]) == 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]) == 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-14.2/contrib/llvm-project/compiler-rt/lib/asan_abi/
H A Dasan_abi_shim.cpp72 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-14.2/contrib/llvm-project/compiler-rt/lib/tsan/rtl/
H A Dtsan_interface.inc21 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 Dtsan_interface_java.cpp49 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 Dtsan_rtl_mutex.cpp47 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-14.2/sys/ddb/
H A Ddb_examine.c113 addr += size; in db_examine()
118 addr += size; in db_examine()
123 addr += size; in db_examine()
128 addr += size; in db_examine()
133 addr += size; in db_examine()
143 addr += 1; in db_examine()
168 addr = db_disasm(addr, false); in db_examine()
171 addr = db_disasm(addr, true); in db_examine()
182 db_next = addr; in db_examine()
256 db_addr_t addr; in db_search_cmd() local
[all …]
/freebsd-14.2/tests/sys/netinet/
H A Dso_reuseport_lb_test.c71 error = connect(sd, addr, addr->sa_len); in lb_simple_accept_loop()
140 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
141 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
145 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
157 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
158 addr.sin_len = sizeof(addr); in ATF_TC_BODY()
196 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
197 addr.sin6_len = sizeof(addr); in ATF_TC_BODY()
201 error = bind(sds[0], (const struct sockaddr *)&addr, sizeof(addr)); in ATF_TC_BODY()
213 memset(&addr, 0, sizeof(addr)); in ATF_TC_BODY()
[all …]
/freebsd-14.2/contrib/jemalloc/src/
H A Dpages.c57 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-14.2/stand/libsa/
H A Dsmbios.c143 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-14.2/contrib/llvm-project/clang/lib/Headers/
H A Davx512pfintrin.h19 (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-14.2/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()
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-14.2/usr.sbin/ppp/
H A Dcbcp.c250 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 Diface.c178 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 …]
H A Dncpaddr.c195 switch (addr->ncpaddr_family) { in ncpaddr_isdefault()
218 switch (addr->ncpaddr_family) { in ncpaddr_equal()
257 addr->ncpaddr_family = AF_INET; in ncpaddr_setip4addr()
273 addr->ncpaddr_family = AF_INET; in ncpaddr_setip4()
274 addr->ncpaddr_ip4addr = ip; in ncpaddr_setip4()
282 *ip = addr->ncpaddr_ip4addr; in ncpaddr_getip4()
291 addr->ncpaddr_ip6addr = *ip6; in ncpaddr_setip6()
299 *ip6 = addr->ncpaddr_ip6addr; in ncpaddr_getip6()
404 return ncpaddr_ntowa(addr); in ncpaddr_ntoa()
847 struct ncpaddr addr; in ncprange_ntoa() local
[all …]
/freebsd-14.2/sys/contrib/dev/rtw88/
H A Dhci.h121 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-14.2/sys/powerpc/powerpc/
H A Dbus_machdep.c83 earlyboot_mappings[earlyboot_map_idx].addr = addr; in bs_gen_map()
188 res = *addr; in native_bs_rs_1()
201 res = *addr; in native_bs_rs_2()
214 res = *addr; in native_bs_rs_4()
227 res = *addr; in native_bs_rs_8()
302 *addr = val; in native_bs_ws_1()
313 *addr = val; in native_bs_ws_2()
324 *addr = val; in native_bs_ws_4()
335 *addr = val; in native_bs_ws_8()
502 res = *addr; in swapped_bs_rs_1()
[all …]
/freebsd-14.2/sys/arm/arm/
H A Dmachdep_ptrace.c233 addr += 8; in arm_predict_branch()
272 addr = pc + 8 + (addr << 2); in arm_predict_branch()
273 error = read_int(cookie, addr, &addr); in arm_predict_branch()
274 *new_pc = addr; in arm_predict_branch()
289 error = read_int(cookie, addr, &addr); in arm_predict_branch()
290 *new_pc = addr; in arm_predict_branch()
302 addr = addr - 0; in arm_predict_branch()
305 addr = addr + 0 + ((nregs - 1) << 2); in arm_predict_branch()
308 addr = addr - 4; in arm_predict_branch()
311 addr = addr + 4 + ((nregs - 1) << 2); in arm_predict_branch()
[all …]
/freebsd-14.2/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-14.2/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-14.2/contrib/llvm-project/compiler-rt/lib/tsan/go/
H A Dtsan_go.cpp58 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-14.2/sys/vm/
H A Dvm_kern.c157 return (addr); in kva_alloc()
178 return (addr); in kva_alloc_aligned()
311 void *addr; in kmem_alloc_attr_domainset() local
322 return (addr); in kmem_alloc_attr_domainset()
366 tmp = addr; in kmem_alloc_contig_domain()
395 void *addr; in kmem_alloc_contig_domainset() local
406 return (addr); in kmem_alloc_contig_domainset()
487 void *addr; in kmem_malloc_domainset() local
497 return (addr); in kmem_malloc_domainset()
577 for (start = addr, end = addr + size; addr < end; addr = next) { in kmem_back()
[all …]
/freebsd-14.2/usr.sbin/acpi/acpidump/
H A Dacpi_user.c134 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-14.2/usr.bin/sdiotool/
H A Dcam_sdio.c34 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 Dlinux_sdio_compat.c59 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 …]

12345678910>>...171