| /netbsd-src/external/cddl/osnet/dist/uts/common/fs/zfs/ |
| H A D | dsl_pool.c | 235 dsl_pool_open_special_dir(dsl_pool_t *dp, const char *name, dsl_dir_t **ddp) in dsl_pool_open_special_dir() argument 240 err = zap_lookup(dp->dp_meta_objset, in dsl_pool_open_special_dir() 241 dsl_dir_phys(dp->dp_root_dir)->dd_child_dir_zapobj, in dsl_pool_open_special_dir() 246 return (dsl_dir_hold_obj(dp, obj, name, dp, ddp)); in dsl_pool_open_special_dir() 252 dsl_pool_t *dp; in dsl_pool_open_impl() local 255 dp = kmem_zalloc(sizeof (dsl_pool_t), KM_SLEEP); in dsl_pool_open_impl() 256 dp->dp_spa = spa; in dsl_pool_open_impl() 257 dp->dp_meta_rootbp = *bp; in dsl_pool_open_impl() 258 rrw_init(&dp->dp_config_rwlock, B_TRUE); in dsl_pool_open_impl() 259 txg_init(dp, txg); in dsl_pool_open_impl() [all …]
|
| /netbsd-src/sys/netinet/ |
| H A D | dccp_usrreq.c | 191 struct dccpcb *dp; in dccp_input() local 411 dp = intodccpcb(inp); in dccp_input() 412 if (dp == NULL) { in dccp_input() 418 if (dp->state == DCCPS_CLOSED) { in dccp_input() 421 dccp_output(dp, DCCP_TYPE_RESET + 2); in dccp_input() 430 DCCP_DEBUG((LOG_INFO, "so->options & SO_ACCEPTCONN! dp->state = %i\n", dp->state)); in dccp_input() 464 dp = inp->inp_ppcb; in dccp_input() 466 dp->state = DCCPS_LISTEN; in dccp_input() 467 dp->who = DCCP_SERVER; in dccp_input() 468 dp->cslen = ((struct dccpcb *)oinp->inp_ppcb)->cslen; in dccp_input() [all …]
|
| /netbsd-src/sys/external/bsd/drm2/dist/drm/nouveau/nvkm/engine/disp/ |
| H A D | nouveau_nvkm_engine_disp_dp.c | 44 struct nvkm_dp *dp; member 55 struct nvkm_dp *dp = lt->dp; in nvkm_dp_train_sense() local 58 if (dp->dpcd[DPCD_RC0E_AUX_RD_INTERVAL]) in nvkm_dp_train_sense() 59 mdelay(dp->dpcd[DPCD_RC0E_AUX_RD_INTERVAL] * 4); in nvkm_dp_train_sense() 63 ret = nvkm_rdaux(dp->aux, DPCD_LS02, lt->stat, 6); in nvkm_dp_train_sense() 68 ret = nvkm_rdaux(dp->aux, DPCD_LS0C, <->pc2stat, 1); in nvkm_dp_train_sense() 71 OUTP_TRACE(&dp->outp, "status %6ph pc2 %02x", in nvkm_dp_train_sense() 74 OUTP_TRACE(&dp->outp, "status %6ph", lt->stat); in nvkm_dp_train_sense() 83 struct nvkm_dp *dp = lt->dp; in nvkm_dp_train_drive() local 84 struct nvkm_ior *ior = dp->outp.ior; in nvkm_dp_train_drive() [all …]
|
| /netbsd-src/sys/arch/arm/iomd/ |
| H A D | iomd_dma.c | 66 dma_go(struct dma_ctrl *dp) in dma_go() argument 72 if (dp->dc_flags & DMA_FL_READY) { in dma_go() 73 dp->dc_flags = DMA_FL_ACTIVE; in dma_go() 74 enable_irq(IRQ_DMACH0 + dp->dc_channel); in dma_go() 80 dma_reset(struct dma_ctrl *dp) in dma_reset() argument 85 dma_dumpdc(dp); in dma_reset() 87 *dp->dc_cr = DMA_CR_CLEAR; in dma_reset() 88 dp->dc_flags = 0; in dma_reset() 89 disable_irq(IRQ_DMACH0 + dp->dc_channel); in dma_reset() 97 dma_setup(struct dma_ctrl *dp, u_char *start, int len, int readp) in dma_setup() argument [all …]
|
| /netbsd-src/crypto/external/bsd/heimdal/dist/lib/roken/ |
| H A D | dirent.c | 112 DIR * dp; in opendir() local 129 dp = malloc(sizeof(*dp)); in opendir() 130 if (dp == NULL) in opendir() 133 memset(dp, 0, sizeof(*dp)); in opendir() 134 dp->magic = DIRINFO_MAGIC; in opendir() 135 dp->cursor = 0; in opendir() 136 dp->n_entries = 0; in opendir() 137 dp->nc_entries = INITIAL_ENTRIES; in opendir() 138 dp->entries = calloc(dp->nc_entries, sizeof(dp->entries[0])); in opendir() 140 if (dp->entries == NULL) { in opendir() [all …]
|
| /netbsd-src/external/bsd/unbound/dist/iterator/ |
| H A D | iter_delegpt.c | 56 struct delegpt* dp=(struct delegpt*)regional_alloc( in delegpt_create() local 57 region, sizeof(*dp)); in delegpt_create() 58 if(!dp) in delegpt_create() 60 memset(dp, 0, sizeof(*dp)); in delegpt_create() 61 return dp; in delegpt_create() 64 struct delegpt* delegpt_copy(struct delegpt* dp, struct regional* region) in delegpt_copy() argument 71 if(!delegpt_set_name(copy, region, dp->name)) in delegpt_copy() 73 copy->bogus = dp->bogus; in delegpt_copy() 74 copy->has_parent_side_NS = dp->has_parent_side_NS; in delegpt_copy() 75 copy->ssl_upstream = dp->ssl_upstream; in delegpt_copy() [all …]
|
| H A D | iter_hints.c | 66 delegpt_free_mlc(s->dp); in hints_stub_free() 92 ah(struct delegpt* dp, const char* sv, const char* ip) in ah() argument 102 if(!delegpt_add_ns_mlc(dp, dname, 0, NULL, UNBOUND_DNS_PORT) || in ah() 104 !delegpt_add_target_mlc(dp, dname, dname_len, in ah() 126 struct delegpt* dp = delegpt_create_mlc((uint8_t*)"\000"); in compile_time_root_prime() local 127 if(!dp) in compile_time_root_prime() 129 dp->has_parent_side_NS = 1; in compile_time_root_prime() 131 if(!ah(dp, "A.ROOT-SERVERS.NET.", "198.41.0.4")) goto failed; in compile_time_root_prime() 132 if(!ah(dp, "B.ROOT-SERVERS.NET.", "199.9.14.201")) goto failed; in compile_time_root_prime() 133 if(!ah(dp, "C.ROOT-SERVERS.NET.", "192.33.4.12")) goto failed; in compile_time_root_prime() [all …]
|
| /netbsd-src/sys/arch/hppa/stand/common/ |
| H A D | dev_hppa.h | 24 #define DEVPATH_PRINT(dp) \ argument 26 (dp)->dp_flags, (dp)->dp_bc[0], (dp)->dp_bc[1], (dp)->dp_bc[2], \ 27 (dp)->dp_bc[3], (dp)->dp_bc[4], (dp)->dp_bc[5], (dp)->dp_mod, \ 28 (dp)->dp_layers[0], (dp)->dp_layers[1], (dp)->dp_layers[2], \ 29 (dp)->dp_layers[3], (dp)->dp_layers[4], (dp)->dp_layers[5]); 30 #define PZDEV_PRINT(dp) \ argument 33 (dp)->pz_flags, (dp)->pz_bc[0], (dp)->pz_bc[1], (dp)->pz_bc[2], \ 34 (dp)->pz_bc[3], (dp)->pz_bc[4], (dp)->pz_bc[5], (dp)->pz_mod, \ 35 (dp)->pz_layers[0], (dp)->pz_layers[1], (dp)->pz_layers[2], \ 36 (dp)->pz_layers[3], (dp)->pz_layers[4], (dp)->pz_layers[5], \ [all …]
|
| /netbsd-src/external/cddl/osnet/dist/lib/libdtrace/common/ |
| H A D | dt_sugar.c | 88 dt_sugar_append_clause(dt_sugar_parse_t *dp, dt_node_t *clause) in dt_sugar_append_clause() argument 90 dp->dtsp_clause_list = dt_node_link(dp->dtsp_clause_list, clause); in dt_sugar_append_clause() 97 dt_sugar_prepend_clause(dt_sugar_parse_t *dp, dt_node_t *clause) in dt_sugar_prepend_clause() argument 99 dp->dtsp_clause_list = dt_node_link(clause, dp->dtsp_clause_list); in dt_sugar_prepend_clause() 142 dt_sugar_new_condition_impl(dt_sugar_parse_t *dp, in dt_sugar_new_condition_impl() argument 171 return (dt_node_clause(dp->dtsp_pdescs, newpred, body)); in dt_sugar_new_condition_impl() 180 dt_sugar_new_condition(dt_sugar_parse_t *dp, dt_node_t *pred, int condid) in dt_sugar_new_condition() argument 182 dp->dtsp_num_conditions++; in dt_sugar_new_condition() 183 dt_sugar_append_clause(dp, dt_sugar_new_condition_impl(dp, in dt_sugar_new_condition() 184 pred, condid, dp->dtsp_num_conditions)); in dt_sugar_new_condition() [all …]
|
| /netbsd-src/external/gpl3/gcc.old/dist/libhsail-rt/rt/ |
| H A D | workitems.c | 265 wg.private_segment_total_size = context->dp->private_segment_size * wg_size; in phsa_execute_wi_gang() 315 wi->wg_size_x = context->dp->workgroup_size_x; in phsa_execute_wi_gang() 316 wi->wg_size_y = context->dp->workgroup_size_y; in phsa_execute_wi_gang() 317 wi->wg_size_z = context->dp->workgroup_size_z; in phsa_execute_wi_gang() 357 hsa_kernel_dispatch_packet_t *dp = context->dp; in phsa_spawn_work_items() local 366 sat_wg_size_x = MIN (dp->workgroup_size_x, dp->grid_size_x); in phsa_spawn_work_items() 367 sat_wg_size_y = MIN (dp->workgroup_size_y, dp->grid_size_y); in phsa_spawn_work_items() 368 sat_wg_size_z = MIN (dp->workgroup_size_z, dp->grid_size_z); in phsa_spawn_work_items() 372 wi_total = (uint64_t) dp->grid_size_x in phsa_spawn_work_items() 373 * (dp->grid_size_y > 0 ? dp->grid_size_y : 1) in phsa_spawn_work_items() [all …]
|
| /netbsd-src/bin/csh/ |
| H A D | dir.c | 79 struct directory *dp; in dinit() local 131 dp = xcalloc(1, sizeof(*dp)); in dinit() 132 dp->di_name = cp; in dinit() 133 dp->di_count = 0; in dinit() 134 dhead.di_next = dhead.di_prev = dp; in dinit() 135 dp->di_next = dp->di_prev = &dhead; in dinit() 137 dnewcwd(dp); in dinit() 141 dset(Char *dp) in dset() argument 151 vec[0] = Strsave(dp); in dset() 154 Setenv(STRPWD, dp); in dset() [all …]
|
| /netbsd-src/external/mpl/dhcp/dist/omapip/ |
| H A D | alloc.c | 69 struct dmalloc_preamble *dp; in dmalloc() local 98 dp = (struct dmalloc_preamble *)foo; in dmalloc() 99 dp -> prev = dmalloc_list; in dmalloc() 101 dmalloc_list -> next = dp; in dmalloc() 102 dmalloc_list = dp; in dmalloc() 103 dp -> next = (struct dmalloc_preamble *)0; in dmalloc() 104 dp -> size = size; in dmalloc() 105 dp -> file = file; in dmalloc() 106 dp -> line = line; in dmalloc() 107 dp -> generation = dmalloc_generation++; in dmalloc() [all …]
|
| /netbsd-src/games/monop/ |
| H A D | cards.c | 207 set_up(DECK *dp) in set_up() argument 212 dp->cards = calloc((size_t)dp->num_cards, sizeof(dp->cards[0])); in set_up() 213 if (dp->cards == NULL) in set_up() 216 for (i = 0; i < dp->num_cards; i++) in set_up() 217 dp->cards[i] = i; in set_up() 219 dp->top_card = 0; in set_up() 220 dp->gojf_used = FALSE; in set_up() 222 for (i = 0; i < dp->num_cards; i++) { in set_up() 225 r1 = roll(1, dp->num_cards) - 1; in set_up() 226 r2 = roll(1, dp->num_cards) - 1; in set_up() [all …]
|
| /netbsd-src/sbin/fsck_ext2fs/ |
| H A D | dir.c | 153 struct ext2fs_direct *dp; in dirscan() local 174 for (dp = fsck_readdir(idesc); dp != NULL; dp = fsck_readdir(idesc)) { in dirscan() 175 dsize = fs2h16(dp->e2d_reclen); in dirscan() 176 memcpy(dbuf, dp, (size_t)dsize); in dirscan() 200 struct ext2fs_direct *dp, *ndp; in fsck_readdir() local 208 dp = (struct ext2fs_direct *)(bp->b_un.b_buf + idesc->id_loc); in fsck_readdir() 209 if (dircheck(idesc, dp)) in fsck_readdir() 215 dp = (struct ext2fs_direct *)(bp->b_un.b_buf + idesc->id_loc); in fsck_readdir() 216 dp->e2d_reclen = h2fs16(sblock.e2fs_bsize); in fsck_readdir() 217 dp->e2d_ino = 0; in fsck_readdir() [all …]
|
| /netbsd-src/sbin/fsck_ffs/ |
| H A D | dir.c | 170 struct direct *dp; in dirscan() local 198 for (off = 0; off < blksiz; off += iswap16(dp->d_reclen)) { in dirscan() 199 dp = (struct direct *)(bp->b_un.b_buf + off); in dirscan() 200 dp->d_ino = bswap32(dp->d_ino); in dirscan() 201 dp->d_reclen = bswap16(dp->d_reclen); in dirscan() 203 u_int8_t tmp = dp->d_namlen; in dirscan() 204 dp->d_namlen = dp->d_type; in dirscan() 205 dp->d_type = tmp; in dirscan() 207 if (dp->d_reclen == 0) in dirscan() 216 for (dp = fsck_readdir(idesc); dp != NULL; dp = fsck_readdir(idesc)) { in dirscan() [all …]
|
| /netbsd-src/sys/arch/alpha/eisa/ |
| H A D | eisa_machdep.c | 199 eisa_parse_mem(struct ecu_func *ecuf, uint8_t *dp) in eisa_parse_mem() argument 206 ecum->ecum_mem.ecm_isram = dp[0] & 0x1; in eisa_parse_mem() 207 ecum->ecum_mem.ecm_unitsize = dp[1] & 0x3; in eisa_parse_mem() 208 ecum->ecum_mem.ecm_decode = (dp[1] >> 2) & 0x3; in eisa_parse_mem() 210 (dp[2] | (dp[3] << 8) | (dp[4] << 16)) << 8; in eisa_parse_mem() 211 ecum->ecum_mem.ecm_size = (dp[5] | (dp[6] << 8)) << 10; in eisa_parse_mem() 223 if ((dp[0] & 0x80) == 0) in eisa_parse_mem() 225 dp += ECUF_MEM_ENTRY_SIZE; in eisa_parse_mem() 230 eisa_parse_irq(struct ecu_func *ecuf, uint8_t *dp) in eisa_parse_irq() argument 237 ecui->ecui_irq.eci_irq = dp[0] & 0xf; in eisa_parse_irq() [all …]
|
| /netbsd-src/external/gpl2/xcvs/dist/lib/ |
| H A D | vasnprintf.c | 151 DIRECTIVE *dp; in VASNPRINTF() local 219 for (cp = format, i = 0, dp = &d.dir[0]; ; cp = dp->dir_end, i++, dp++) in VASNPRINTF() 221 if (cp != dp->dir_start) in VASNPRINTF() 223 size_t n = dp->dir_start - cp; in VASNPRINTF() 234 if (dp->conversion == '%') in VASNPRINTF() 238 if (!(dp->arg_index == ARG_NONE)) in VASNPRINTF() 247 if (!(dp->arg_index != ARG_NONE)) in VASNPRINTF() 250 if (dp->conversion == 'n') in VASNPRINTF() 252 switch (a.arg[dp->arg_index].type) in VASNPRINTF() 255 *a.arg[dp->arg_index].a.a_count_schar_pointer = length; in VASNPRINTF() [all …]
|
| /netbsd-src/external/gpl2/texinfo/dist/intl/ |
| H A D | vasnprintf.c | 141 DIRECTIVE *dp; in VASNPRINTF() local 209 for (cp = format, i = 0, dp = &d.dir[0]; ; cp = dp->dir_end, i++, dp++) in VASNPRINTF() 211 if (cp != dp->dir_start) in VASNPRINTF() 213 size_t n = dp->dir_start - cp; in VASNPRINTF() 224 if (dp->conversion == '%') in VASNPRINTF() 228 if (!(dp->arg_index == ARG_NONE)) in VASNPRINTF() 237 if (!(dp->arg_index != ARG_NONE)) in VASNPRINTF() 240 if (dp->conversion == 'n') in VASNPRINTF() 242 switch (a.arg[dp->arg_index].type) in VASNPRINTF() 245 *a.arg[dp->arg_index].a.a_count_schar_pointer = length; in VASNPRINTF() [all …]
|
| /netbsd-src/sbin/dump/ |
| H A D | traverse.c | 62 static int appendextdata(union dinode *dp); 63 static void writeextdata(union dinode *dp, ino_t ino, int added); 65 static void dmpindir(union dinode *dp, ino_t, daddr_t, int, off_t *); 76 blockest(union dinode *dp) in blockest() argument 94 if (DIP(dp, flags) & SF_SNAPSHOT) in blockest() 97 dbtob((u_int64_t)DIP(dp, blocks))), TP_BSIZE); in blockest() 98 sizeest = howmany(ufs_fragroundup(ufsib, DIP(dp, size)), TP_BSIZE); in blockest() 101 if (DIP(dp, size) > ufsib->ufs_bsize * UFS_NDADDR) { in blockest() 111 #define CHANGEDSINCE(dp, t) \ argument 112 (DIP((dp), mtime) >= (t) || DIP((dp), ctime) >= (t)) [all …]
|
| /netbsd-src/external/gpl3/binutils/dist/binutils/ |
| H A D | unwind-ia64.c | 355 #define UNW_DEC_SPILL_MASK(fmt, dp, arg, end) \ argument 359 unsigned const char *imaskp = dp; \ 364 if ((dp + (unw_rlen / 4)) > end) \ 367 (long) (unw_rlen / 4), (long)(end - dp)); \ 381 dp = imaskp; \ 584 unw_decode_x1 (const unsigned char *dp, unsigned int code ATTRIBUTE_UNUSED, in unw_decode_x1() argument 590 if ((end - dp) < 3) in unw_decode_x1() 596 byte1 = *dp++; in unw_decode_x1() 597 t = unw_decode_uleb128 (&dp, end); in unw_decode_x1() 598 off = unw_decode_uleb128 (&dp, end); in unw_decode_x1() [all …]
|
| /netbsd-src/external/gpl3/binutils.old/dist/binutils/ |
| H A D | unwind-ia64.c | 355 #define UNW_DEC_SPILL_MASK(fmt, dp, arg, end) \ argument 359 unsigned const char *imaskp = dp; \ 364 if ((dp + (unw_rlen / 4)) > end) \ 367 (long) (unw_rlen / 4), (long)(end - dp)); \ 381 dp = imaskp; \ 584 unw_decode_x1 (const unsigned char *dp, unsigned int code ATTRIBUTE_UNUSED, in unw_decode_x1() argument 590 if ((end - dp) < 3) in unw_decode_x1() 596 byte1 = *dp++; in unw_decode_x1() 597 t = unw_decode_uleb128 (&dp, end); in unw_decode_x1() 598 off = unw_decode_uleb128 (&dp, end); in unw_decode_x1() [all …]
|
| /netbsd-src/lib/libc/gen/ |
| H A D | disklabel.c | 95 struct disklabel *dp = &disk; in getdiskbyname() local 113 cq = dp->d_typename; in getdiskbyname() 115 while (cq < dp->d_typename + sizeof(dp->d_typename) - 1 && in getdiskbyname() 122 cgetstr(buf, "b0", &dp->d_boot0); in getdiskbyname() 123 cgetstr(buf, "b1", &dp->d_boot1); in getdiskbyname() 127 dp->d_flags |= D_REMOVABLE; in getdiskbyname() 129 dp->d_flags |= D_RAMDISK; in getdiskbyname() 133 dp->d_flags |= D_BADSECT; in getdiskbyname() 140 getnumdflt(dp->d_secsize, "se", DEV_BSIZE); in getdiskbyname() 141 getnum(dp->d_ntracks, "nt"); in getdiskbyname() [all …]
|
| /netbsd-src/external/bsd/am-utils/dist/fsinfo/ |
| H A D | wr_fstab.c | 52 static void write_aix1_dkfstab(FILE *ef, disk_fs *dp); 54 static void write_aix3_dkfstab(FILE *ef, disk_fs *dp); 58 static void write_generic_dkfstab(FILE *ef, disk_fs *dp); 60 static void write_ultrix_dkfstab(FILE *ef, disk_fs *dp); 67 void (*op_fstab) (FILE *ef, disk_fs *dp); 101 write_aix1_dkfstab(FILE *ef, disk_fs *dp) in write_aix1_dkfstab() argument 103 char *hp = xstrdup(dp->d_host->h_hostname); in write_aix1_dkfstab() 110 dp->d_mountpt, in write_aix1_dkfstab() 111 dp->d_dev, in write_aix1_dkfstab() 112 dp->d_fstype, in write_aix1_dkfstab() [all …]
|
| /netbsd-src/sbin/fsck_lfs/ |
| H A D | dir.c | 133 LFS_DIRHEADER *dp; in dirscan() local 153 for (dp = fsck_readdir(vp, idesc); dp != NULL; in dirscan() 154 dp = fsck_readdir(vp, idesc)) { in dirscan() 155 dsize = lfs_dir_getreclen(fs, dp); in dirscan() 156 memcpy(dbuf, dp, (size_t) dsize); in dirscan() 177 LFS_DIRHEADER *dp, *ndp; in fsck_readdir() local 185 dp = (LFS_DIRHEADER *) (bp->b_data + idesc->id_loc); in fsck_readdir() 186 if (dircheck(idesc, dp)) in fsck_readdir() 193 dp = (LFS_DIRHEADER *) (bp->b_data + idesc->id_loc); in fsck_readdir() 194 lfs_dir_setino(fs, dp, 0); in fsck_readdir() [all …]
|
| /netbsd-src/external/gpl2/gettext/dist/gettext-runtime/libasprintf/ |
| H A D | vasnprintf.c | 137 DIRECTIVE *dp; in VASNPRINTF() local 205 for (cp = format, i = 0, dp = &d.dir[0]; ; cp = dp->dir_end, i++, dp++) in VASNPRINTF() 207 if (cp != dp->dir_start) in VASNPRINTF() 209 size_t n = dp->dir_start - cp; in VASNPRINTF() 220 if (dp->conversion == '%') in VASNPRINTF() 224 if (!(dp->arg_index == ARG_NONE)) in VASNPRINTF() 233 if (!(dp->arg_index != ARG_NONE)) in VASNPRINTF() 236 if (dp->conversion == 'n') in VASNPRINTF() 238 switch (a.arg[dp->arg_index].type) in VASNPRINTF() 241 *a.arg[dp->arg_index].a.a_count_schar_pointer = length; in VASNPRINTF() [all …]
|