/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
|