| /freebsd/sys/compat/linuxkpi/common/include/linux/ |
| H A D | io.h | 139 readb(const volatile void *addr) in readb()
148 #define readb(addr) readb(addr) argument
162 readw(const volatile void *addr) in readw()
171 #define readw(addr) readw(addr) argument
185 readl(const volatile void *addr) in readl()
194 #define readl(addr) readl(addr) argument
210 readq(const volatile void *addr) in readq()
219 #define readq(addr) readq(addr) argument
303 ioread8(const volatile void *addr) in ioread8()
512 void *addr = NULL; in memremap() local
[all …]
|
| H A D | io-64-nonatomic-lo-hi.h | 33 lo_hi_readq(const volatile void *addr) in lo_hi_readq()
47 lo_hi_writeq(uint64_t v, volatile void *addr) in lo_hi_writeq()
58 #define readq(addr) lo_hi_readq(addr) argument
62 #define writeq(v, addr) lo_hi_writeq(v, addr) argument
|
| /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()
75 void __asan_report_load2(uptr addr) { in __asan_report_load2()
78 void __asan_report_load4(uptr addr) { in __asan_report_load4()
81 void __asan_report_load8(uptr addr) { in __asan_report_load8()
84 void __asan_report_load16(uptr addr) { in __asan_report_load16()
90 void __asan_report_store1(uptr addr) { in __asan_report_store1()
93 void __asan_report_store2(uptr addr) { in __asan_report_store2()
96 void __asan_report_store4(uptr addr) { in __asan_report_store4()
99 void __asan_report_store8(uptr addr) { in __asan_report_store8()
102 void __asan_report_store16(uptr addr) { in __asan_report_store16()
[all …]
|
| /freebsd/crypto/openssl/include/openssl/ |
| H A D | params.h | 31 # define OSSL_PARAM_int(key, addr) \ argument
33 # define OSSL_PARAM_uint(key, addr) \ argument
36 # define OSSL_PARAM_long(key, addr) \ argument
38 # define OSSL_PARAM_ulong(key, addr) \ argument
41 # define OSSL_PARAM_int32(key, addr) \ argument
43 # define OSSL_PARAM_uint32(key, addr) \ argument
46 # define OSSL_PARAM_int64(key, addr) \ argument
48 # define OSSL_PARAM_uint64(key, addr) \ argument
51 # define OSSL_PARAM_size_t(key, addr) \ argument
53 # define OSSL_PARAM_time_t(key, addr) \ argument
[all …]
|
| /freebsd/contrib/llvm-project/clang/lib/Headers/ |
| H A D | avx512pfintrin.h | 17 #define _mm512_mask_prefetch_i32gather_pd(index, mask, addr, scale, hint) \ argument
22 #define _mm512_prefetch_i32gather_pd(index, addr, scale, hint) \ argument
27 #define _mm512_mask_prefetch_i32gather_ps(index, mask, addr, scale, hint) \ argument
32 #define _mm512_prefetch_i32gather_ps(index, addr, scale, hint) \ argument
37 #define _mm512_mask_prefetch_i64gather_pd(index, mask, addr, scale, hint) \ argument
42 #define _mm512_prefetch_i64gather_pd(index, addr, scale, hint) \ argument
51 #define _mm512_prefetch_i64gather_ps(index, addr, scale, hint) \ argument
55 #define _mm512_prefetch_i32scatter_pd(addr, index, scale, hint) \ argument
65 #define _mm512_prefetch_i32scatter_ps(addr, index, scale, hint) \ argument
74 #define _mm512_prefetch_i64scatter_pd(addr, index, scale, hint) \ argument
[all …]
|
| /freebsd/sys/powerpc/powerpc/ |
| H A D | bus_machdep.c | 56 bus_addr_t addr; member
189 volatile uint8_t *addr; in native_bs_rs_1() local
202 volatile uint16_t *addr; in native_bs_rs_2() local
215 volatile uint32_t *addr; in native_bs_rs_4() local
228 volatile uint64_t *addr; in native_bs_rs_8() local
304 volatile uint8_t *addr; in native_bs_ws_1() local
315 volatile uint16_t *addr; in native_bs_ws_2() local
326 volatile uint32_t *addr; in native_bs_ws_4() local
337 volatile uint64_t *addr; in native_bs_ws_8() local
503 volatile uint8_t *addr; in swapped_bs_rs_1() local
[all …]
|
| /freebsd/usr.bin/sdiotool/ |
| H A D | linux_sdio_compat.c | 58 u8 sdio_readb(struct sdio_func *func, unsigned int addr, int *err_ret) { in sdio_readb()
62 unsigned char sdio_f0_readb(struct sdio_func *func, unsigned int addr, int *err_ret) { in sdio_f0_readb()
66 u16 sdio_readw(struct sdio_func *func, unsigned int addr, int *err_ret) { in sdio_readw()
70 u32 sdio_readl(struct sdio_func *func, unsigned int addr, int *err_ret) { in sdio_readl()
75 unsigned int addr, int *err_ret) { in sdio_writeb()
82 unsigned int addr, int *err_ret) in sdio_f0_writeb()
93 unsigned int addr, int *err_ret) { in sdio_writew()
98 unsigned int addr, int *err_ret) { in sdio_writel()
|
| /freebsd/contrib/jemalloc/src/ |
| H A D | pages.c | 130 os_pages_unmap(void *addr, size_t size) { in os_pages_unmap()
243 pages_unmap(void *addr, size_t size) { in pages_unmap()
284 pages_commit(void *addr, size_t size) { in pages_commit()
289 pages_decommit(void *addr, size_t size) { in pages_decommit()
294 pages_purge_lazy(void *addr, size_t size) { in pages_purge_lazy()
329 pages_purge_forced(void *addr, size_t size) { in pages_purge_forced()
362 pages_huge(void *addr, size_t size) { in pages_huge()
367 pages_huge_unaligned(void *addr, size_t size) { in pages_huge_unaligned()
386 pages_nohuge(void *addr, size_t size) { in pages_nohuge()
396 pages_dontdump(void *addr, size_t size) { in pages_dontdump()
[all …]
|
| /freebsd/usr.sbin/ppp/ |
| H A D | ncpaddr.c | 181 ncpaddr_init(struct ncpaddr *addr) in ncpaddr_init()
187 ncpaddr_isset(const struct ncpaddr *addr) in ncpaddr_isset()
193 ncpaddr_isdefault(const struct ncpaddr *addr) in ncpaddr_isdefault()
236 ncpaddr_copy(struct ncpaddr *addr, const struct ncpaddr *from) in ncpaddr_copy()
255 ncpaddr_setip4addr(struct ncpaddr *addr, u_int32_t ip) in ncpaddr_setip4addr()
262 ncpaddr_getip4addr(const struct ncpaddr *addr, u_int32_t *ip) in ncpaddr_getip4addr()
271 ncpaddr_setip4(struct ncpaddr *addr, struct in_addr ip) in ncpaddr_setip4()
278 ncpaddr_getip4(const struct ncpaddr *addr, struct in_addr *ip) in ncpaddr_getip4()
368 ncpaddr_ntowa(const struct ncpaddr *addr) in ncpaddr_ntowa()
402 ncpaddr_ntoa(const struct ncpaddr *addr) in ncpaddr_ntoa()
[all …]
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/tsan/rtl/ |
| H A D | tsan_interface_java.cpp | 40 MBlock *JavaHeapBlock(uptr addr, uptr *start) { in JavaHeapBlock()
162 void __tsan_java_mutex_lock(jptr addr) { in __tsan_java_mutex_lock()
174 void __tsan_java_mutex_unlock(jptr addr) { in __tsan_java_mutex_unlock()
184 void __tsan_java_mutex_read_lock(jptr addr) { in __tsan_java_mutex_read_lock()
196 void __tsan_java_mutex_read_unlock(jptr addr) { in __tsan_java_mutex_read_unlock()
206 void __tsan_java_mutex_lock_rec(jptr addr, int rec) { in __tsan_java_mutex_lock_rec()
220 int __tsan_java_mutex_unlock_rec(jptr addr) { in __tsan_java_mutex_unlock_rec()
230 void __tsan_java_acquire(jptr addr) { in __tsan_java_acquire()
240 void __tsan_java_release(jptr addr) { in __tsan_java_release()
250 void __tsan_java_release_store(jptr addr) { in __tsan_java_release_store()
|
| H A D | tsan_interface.cpp | 29 void __tsan_read16_pc(void *addr, void *pc) { in __tsan_read16_pc()
36 void __tsan_write16_pc(void *addr, void *pc) { in __tsan_write16_pc()
45 void __tsan_unaligned_read16(const void *addr) { in __tsan_unaligned_read16()
52 void __tsan_unaligned_write16(void *addr) { in __tsan_unaligned_write16()
86 void __tsan_acquire(void *addr) { in __tsan_acquire()
90 void __tsan_release(void *addr) { in __tsan_release()
|
| /freebsd/sys/dev/rtwn/usb/ |
| H A D | rtwn_usb_reg.c | 87 rtwn_usb_write_region_1(struct rtwn_softc *sc, uint16_t addr, uint8_t *buf, in rtwn_usb_write_region_1()
101 rtwn_usb_write_1(struct rtwn_softc *sc, uint16_t addr, uint8_t val) in rtwn_usb_write_1()
107 rtwn_usb_write_2(struct rtwn_softc *sc, uint16_t addr, uint16_t val) in rtwn_usb_write_2()
114 rtwn_usb_write_4(struct rtwn_softc *sc, uint16_t addr, uint32_t val) in rtwn_usb_write_4()
121 rtwn_usb_read_region_1(struct rtwn_softc *sc, uint16_t addr, uint8_t *buf, in rtwn_usb_read_region_1()
135 rtwn_usb_read_1(struct rtwn_softc *sc, uint16_t addr) in rtwn_usb_read_1()
145 rtwn_usb_read_2(struct rtwn_softc *sc, uint16_t addr) in rtwn_usb_read_2()
155 rtwn_usb_read_4(struct rtwn_softc *sc, uint16_t addr) in rtwn_usb_read_4()
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/asan/ |
| H A D | asan_descriptions.cpp | 71 static bool GetShadowKind(uptr addr, ShadowKind *shadow_kind) { in GetShadowKind()
85 bool DescribeAddressIfShadow(uptr addr) { in DescribeAddressIfShadow()
126 static void PrintHeapChunkAccess(uptr addr, const ChunkAccess &descr) { in PrintHeapChunkAccess()
155 bool GetHeapAddressInformation(uptr addr, uptr access_size, in GetHeapAddressInformation()
180 bool DescribeAddressIfHeap(uptr addr, uptr access_size) { in DescribeAddressIfHeap()
193 bool GetStackAddressInformation(uptr addr, uptr access_size, in GetStackAddressInformation()
268 bool DescribeAddressIfStack(uptr addr, uptr access_size) { in DescribeAddressIfStack()
301 bool GetGlobalAddressInformation(uptr addr, uptr access_size, in GetGlobalAddressInformation()
311 bool DescribeAddressIfGlobal(uptr addr, uptr access_size, in DescribeAddressIfGlobal()
439 AddressDescription::AddressDescription(uptr addr, uptr access_size, in AddressDescription()
[all …]
|
| /freebsd/contrib/llvm-project/compiler-rt/lib/tsan/go/ |
| H A D | tsan_go.cpp | 26 bool IsExpectedReport(uptr addr, uptr size) { in IsExpectedReport()
52 SymbolizedStack *SymbolizeCode(uptr addr) { in SymbolizeCode()
81 uptr addr; member
91 ReportLocation *SymbolizeData(uptr addr) { in SymbolizeData()
165 void __tsan_map_shadow(uptr addr, uptr size) { in __tsan_map_shadow()
169 void __tsan_read(ThreadState *thr, void *addr, void *pc) { in __tsan_read()
181 void __tsan_write(ThreadState *thr, void *addr, void *pc) { in __tsan_write()
240 void __tsan_acquire(ThreadState *thr, void *addr) { in __tsan_acquire()
244 void __tsan_release_acquire(ThreadState *thr, void *addr) { in __tsan_release_acquire()
248 void __tsan_release(ThreadState *thr, void *addr) { in __tsan_release()
[all …]
|
| /freebsd/contrib/ofed/libmlx4/ |
| H A D | mmio.h | 77 #define mmio_writeb(addr, value) \ argument
79 #define mmio_writew(addr, value) \ argument
81 #define mmio_writel(addr, value) \ argument
83 #define mmio_writeq(addr, value) \ argument
85 #define mmio_write(addr, value, length) \ argument
88 #define mmio_readb(addr, value) \ argument
90 #define mmio_readw(addr, value) \ argument
92 #define mmio_readl(addr, value) \ argument
94 #define mmio_readq(addr, value) \ argument
96 #define mmio_read(addr, value, length) \ argument
|
| /freebsd/sys/dev/rtwn/pci/ |
| H A D | rtwn_pci_reg.c | 51 rtwn_pci_write_1(struct rtwn_softc *sc, uint16_t addr, uint8_t val) in rtwn_pci_write_1()
61 rtwn_pci_write_2(struct rtwn_softc *sc, uint16_t addr, uint16_t val) in rtwn_pci_write_2()
72 rtwn_pci_write_4(struct rtwn_softc *sc, uint16_t addr, uint32_t val) in rtwn_pci_write_4()
83 rtwn_pci_read_1(struct rtwn_softc *sc, uint16_t addr) in rtwn_pci_read_1()
91 rtwn_pci_read_2(struct rtwn_softc *sc, uint16_t addr) in rtwn_pci_read_2()
101 rtwn_pci_read_4(struct rtwn_softc *sc, uint16_t addr) in rtwn_pci_read_4()
|
| /freebsd/sys/dev/etherswitch/arswitch/ |
| H A D | arswitch_reg.c | 65 arswitch_split_setpage(device_t dev, uint32_t addr, uint16_t *phy, in arswitch_split_setpage()
88 arswitch_readreg16(device_t dev, int addr) in arswitch_readreg16()
100 arswitch_writereg16(device_t dev, int addr, int data) in arswitch_writereg16()
165 arswitch_readreg(device_t dev, int addr) in arswitch_readreg()
174 arswitch_writereg(device_t dev, int addr, int value) in arswitch_writereg()
190 arswitch_readreg_lsb(device_t dev, int addr) in arswitch_readreg_lsb()
197 arswitch_readreg_msb(device_t dev, int addr) in arswitch_readreg_msb()
204 arswitch_writereg_lsb(device_t dev, int addr, int data) in arswitch_writereg_lsb()
211 arswitch_writereg_msb(device_t dev, int addr, int data) in arswitch_writereg_msb()
218 arswitch_modifyreg(device_t dev, int addr, int mask, int set) in arswitch_modifyreg()
[all …]
|
| /freebsd/sys/contrib/dev/rtw88/ |
| H A D | hci.h | 87 static inline u8 rtw_read8(struct rtw_dev *rtwdev, u32 addr) in rtw_read8()
92 static inline u16 rtw_read16(struct rtw_dev *rtwdev, u32 addr) in rtw_read16()
97 static inline u32 rtw_read32(struct rtw_dev *rtwdev, u32 addr) in rtw_read32()
102 static inline void rtw_write8(struct rtw_dev *rtwdev, u32 addr, u8 val) in rtw_write8()
167 u32 addr, u32 mask) in rtw_read_rf()
180 u32 addr, u32 mask, u32 data) in rtw_write_rf()
188 rtw_read32_mask(struct rtw_dev *rtwdev, u32 addr, u32 mask) in rtw_read32_mask()
201 rtw_read16_mask(struct rtw_dev *rtwdev, u32 addr, u32 mask) in rtw_read16_mask()
214 rtw_read8_mask(struct rtw_dev *rtwdev, u32 addr, u32 mask) in rtw_read8_mask()
227 rtw_write32_mask(struct rtw_dev *rtwdev, u32 addr, u32 mask, u32 data) in rtw_write32_mask()
[all …]
|
| /freebsd/sys/amd64/amd64/ |
| H A D | fpu.c | 99 xsave32(char *addr, uint64_t mask) in xsave32()
176 fpusave_xsaveopt64(void *addr) in fpusave_xsaveopt64()
182 fpusave_xsaveopt3264(void *addr) in fpusave_xsaveopt3264()
191 fpusave_xsave64(void *addr) in fpusave_xsave64()
197 fpusave_xsave3264(void *addr) in fpusave_xsave3264()
206 fpurestore_xrstor64(void *addr) in fpurestore_xrstor64()
212 fpurestore_xrstor3264(void *addr) in fpurestore_xrstor3264()
221 fpusave_fxsave(void *addr) in fpusave_fxsave()
228 fpurestore_fxrstor(void *addr) in fpurestore_fxrstor()
258 fpususpend(void *addr) in fpususpend()
[all …]
|
| /freebsd/sys/ddb/ |
| H A D | db_break.c | 120 db_addr_t addr, int count) in db_set_breakpoint()
149 db_addr_t addr) in db_delete_breakpoint()
173 db_addr_t addr) in db_find_breakpoint()
189 db_find_breakpoint_here(db_addr_t addr) in db_find_breakpoint_here()
206 #define BKPT_WRITE(addr, storage) \ argument
214 #define BKPT_CLEAR(addr, storage) \ argument
286 db_delete_cmd(db_expr_t addr, bool have_addr, db_expr_t count, char *modif) in db_delete_cmd()
297 db_breakpoint_cmd(db_expr_t addr, bool have_addr, db_expr_t count, char *modif) in db_breakpoint_cmd()
311 db_deletehbreak_cmd(db_expr_t addr, bool have_addr, db_expr_t count, in db_deletehbreak_cmd()
330 db_hbreakpoint_cmd(db_expr_t addr, bool have_addr, db_expr_t count, char *modif) in db_hbreakpoint_cmd()
[all …]
|
| H A D | db_pprint.c | 53 db_pprint_int(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_int()
83 db_pprint_struct(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_struct()
165 db_pprint_arr(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_arr()
206 db_pprint_enum(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_enum()
245 db_pprint_ptr(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_ptr()
287 db_pprint_type(db_addr_t addr, struct ctf_type_v3 *type, u_int depth) in db_pprint_type()
343 db_addr_t addr; in db_pprint_symbol_cmd() local
379 db_pprint_struct_cmd(db_expr_t addr, const char *struct_name) in db_pprint_struct_cmd()
402 db_pprint_cmd(db_expr_t addr, bool have_addr, db_expr_t count, char *modif) in db_pprint_cmd()
|
| /freebsd/sys/dev/sdio/ |
| H A D | sdio_subr.c | 73 sdio_set_bool_for_func(device_t dev, uint32_t addr, uint8_t fn, bool enable) in sdio_set_bool_for_func()
118 uint32_t addr; in sdio_set_block_size() local
142 sdio_read_1(struct sdio_func *f, uint32_t addr, int *err) in sdio_read_1()
160 sdio_write_1(struct sdio_func *f, uint32_t addr, uint8_t val, int *err) in sdio_write_1()
170 sdio_read_4(struct sdio_func *f, uint32_t addr, int *err) in sdio_read_4()
189 sdio_write_4(struct sdio_func *f, uint32_t addr, uint32_t val, int *err) in sdio_write_4()
200 sdio_f0_read_1(struct sdio_func *f, uint32_t addr, int *err) in sdio_f0_read_1()
218 sdio_f0_write_1(struct sdio_func *f, uint32_t addr, uint8_t val, int *err) in sdio_f0_write_1()
|
| /freebsd/sys/compat/linuxkpi/common/include/net/ |
| H A D | ipv6.h | 44 #define ipv6_addr_loopback(addr) IN6_IS_ADDR_LOOPBACK(addr) argument
45 #define ipv6_addr_any(addr) IN6_IS_ADDR_UNSPECIFIED(addr) argument
51 ipv6_ib_mc_map(const struct in6_addr *addr, const unsigned char *broadcast, in ipv6_ib_mc_map()
70 static inline void __ipv6_addr_set_half(__be32 *addr, __be32 wh, __be32 wl) in __ipv6_addr_set_half()
89 static inline void ipv6_addr_set(struct in6_addr *addr, in ipv6_addr_set()
97 static inline void ipv6_addr_set_v4mapped(const __be32 addr, in ipv6_addr_set_v4mapped()
|
| /freebsd/contrib/libpcap/ |
| H A D | fad-getad.c | 105 #define SA_LEN(addr) ((addr)->sa_len) argument
109 get_sa_len(struct sockaddr *addr) in get_sa_len()
132 #define SA_LEN(addr) (get_sa_len(addr)) argument
134 #define SA_LEN(addr) (sizeof (struct sockaddr)) argument
150 struct sockaddr *addr, *netmask, *broadaddr, *dstaddr; in pcap_findalldevs_interfaces() local
|
| /freebsd/contrib/llvm-project/compiler-rt/include/sanitizer/ |
| H A D | asan_interface.h | 69 #define ASAN_POISON_MEMORY_REGION(addr, size) \ argument
79 #define ASAN_UNPOISON_MEMORY_REGION(addr, size) \ argument
82 #define ASAN_POISON_MEMORY_REGION(addr, size) ((void)(addr), (void)(size)) argument
83 #define ASAN_UNPOISON_MEMORY_REGION(addr, size) ((void)(addr), (void)(size)) argument
|