Home
last modified time | relevance | path

Searched refs:alist (Results 1 – 24 of 24) sorted by relevance

/linux/fs/afs/
A Daddr_list.c24 kfree(alist); in afs_free_addrlist()
36 if (!alist) in afs_put_addrlist()
49 if (alist) { in afs_get_addrlist()
53 return alist; in afs_get_addrlist()
70 if (!alist) in afs_alloc_addrlist()
77 return alist; in afs_alloc_addrlist()
150 if (!alist) in afs_parse_text_addrs()
290 if (alist->nr_addrs >= alist->max_addrs) in afs_merge_fs_addr4()
316 sizeof(alist->addrs[0]) * (alist->nr_addrs - i)); in afs_merge_fs_addr4()
334 if (alist->nr_addrs >= alist->max_addrs) in afs_merge_fs_addr6()
[all …]
A Dvl_rotate.c95 struct afs_addr_list *alist = vc->alist; in afs_select_vlserver() local
179 alist = vc->alist = NULL; in afs_select_vlserver()
247 vc->alist = afs_get_addrlist(alist, afs_alist_trace_get_vlrotate_set); in afs_select_vlserver()
272 vc->alist = alist; in afs_select_vlserver()
282 ASSERT(alist); in afs_select_vlserver()
288 alist = vc->alist = NULL; in afs_select_vlserver()
308 if (alist) { in afs_select_vlserver()
314 alist = vc->alist = NULL; in afs_select_vlserver()
361 if (a == vc->alist) in afs_vl_dump_edestaddrreq()
389 if (vc->alist) { in afs_end_vlserver_operation()
[all …]
A Dserver.c27 const struct afs_addr_list *alist; in afs_find_server() local
43 alist = estate->addresses; in afs_find_server()
170 alist = estate->addresses; in afs_install_server()
180 if (alist->nr_addrs > 0) in afs_install_server()
229 estate->addresses = alist; in afs_alloc_server()
279 struct afs_addr_list *alist; in afs_lookup_server() local
292 if (IS_ERR(alist)) in afs_lookup_server()
293 return ERR_CAST(alist); in afs_lookup_server()
459 afs_fs_give_up_all_callbacks(net, server, &alist->addrs[alist->preferred], NULL); in afs_give_up_callbacks()
630 struct afs_addr_list *alist; in afs_update_server_record() local
[all …]
A Dvl_probe.c49 struct afs_addr_list *alist = call->vl_probe; in afs_vlserver_probe_result() local
92 clear_bit(index, &alist->responded); in afs_vlserver_probe_result()
93 set_bit(index, &alist->probe_failed); in afs_vlserver_probe_result()
104 set_bit(index, &alist->responded); in afs_vlserver_probe_result()
105 clear_bit(index, &alist->probe_failed); in afs_vlserver_probe_result()
123 alist->preferred = index; in afs_vlserver_probe_result()
152 struct afs_addr_list *alist; in afs_do_probe_vlserver() local
171 unprobed = (1UL << alist->nr_addrs) - 1; in afs_do_probe_vlserver()
175 for (i = 0; i < alist->nr_addrs; i++) { in afs_do_probe_vlserver()
177 alist->addrs[i].prio > best_prio) { in afs_do_probe_vlserver()
[all …]
A Dvlclient.c175 struct afs_addr_list *alist; in afs_deliver_vl_get_addrs_u() local
204 if (!alist) in afs_deliver_vl_get_addrs_u()
207 call->ret_alist = alist; in afs_deliver_vl_get_addrs_u()
222 alist = call->ret_alist; in afs_deliver_vl_get_addrs_u()
305 alist = call->ret_alist; in afs_vl_get_addrs_u()
311 return alist; in afs_vl_get_addrs_u()
463 if (!alist) in afs_deliver_yfsvl_get_endpoints()
466 call->ret_alist = alist; in afs_deliver_yfsvl_get_endpoints()
493 alist = call->ret_alist; in afs_deliver_yfsvl_get_endpoints()
667 alist = call->ret_alist; in afs_yfsvl_get_endpoints()
[all …]
A Dvl_list.c94 struct afs_addr_list *alist; in afs_extract_vl_addrs() local
98 alist = afs_alloc_addrlist(nr_addrs); in afs_extract_vl_addrs()
99 if (!alist) in afs_extract_vl_addrs()
102 return alist; in afs_extract_vl_addrs()
117 ret = afs_merge_fs_addr4(net, alist, x[0], port); in afs_extract_vl_addrs()
129 ret = afs_merge_fs_addr6(net, alist, x, port); in afs_extract_vl_addrs()
144 if (alist->nr_ipv4 < alist->nr_addrs) in afs_extract_vl_addrs()
145 alist->preferred = alist->nr_ipv4; in afs_extract_vl_addrs()
148 return alist; in afs_extract_vl_addrs()
152 afs_put_addrlist(alist, afs_alist_trace_put_parse_error); in afs_extract_vl_addrs()
A Daddr_prefs.c466 if (!preflist || !preflist->nr || !alist->nr_addrs || in afs_get_address_preferences_rcu()
467 smp_load_acquire(&alist->addr_pref_version) == preflist->version) in afs_get_address_preferences_rcu()
473 for (i = 0; i < alist->nr_ipv4; i++) { in afs_get_address_preferences_rcu()
474 sa = rxrpc_kernel_remote_addr(alist->addrs[i].peer); in afs_get_address_preferences_rcu()
486 WRITE_ONCE(alist->addrs[i].prio, preflist->prefs[j].prio); in afs_get_address_preferences_rcu()
495 for (; i < alist->nr_addrs; i++) { in afs_get_address_preferences_rcu()
496 sa = rxrpc_kernel_remote_addr(alist->addrs[i].peer); in afs_get_address_preferences_rcu()
508 WRITE_ONCE(alist->addrs[i].prio, preflist->prefs[j].prio); in afs_get_address_preferences_rcu()
514 smp_store_release(&alist->addr_pref_version, preflist->version); in afs_get_address_preferences_rcu()
525 smp_load_acquire(&net->address_pref_version) == alist->addr_pref_version) in afs_get_address_preferences()
[all …]
A Dproc.c338 const struct afs_addr_list *alist; in afs_proc_cell_vlservers_show() local
354 dns_record_sources[alist ? alist->source : entry->source], in afs_proc_cell_vlservers_show()
355 dns_lookup_statuses[alist ? alist->status : entry->status]); in afs_proc_cell_vlservers_show()
356 if (alist) { in afs_proc_cell_vlservers_show()
357 for (i = 0; i < alist->nr_addrs; i++) in afs_proc_cell_vlservers_show()
359 alist->preferred == i ? '>' : '-', in afs_proc_cell_vlservers_show()
429 struct afs_addr_list *alist; in afs_proc_servers_show() local
441 alist = estate->addresses; in afs_proc_servers_show()
456 alist->version, alist->addr_pref_version); in afs_proc_servers_show()
457 for (i = 0; i < alist->nr_addrs; i++) { in afs_proc_servers_show()
[all …]
A Dfs_probe.c141 struct afs_addr_list *alist = estate->addresses; in afs_fileserver_probe_result() local
215 alist->preferred = index; in afs_fileserver_probe_result()
228 rxrpc_kernel_remote_addr(alist->addrs[index].peer), in afs_fileserver_probe_result()
242 struct afs_addr_list *alist; in afs_fs_probe_fileserver() local
262 alist = estate->addresses; in afs_fs_probe_fileserver()
264 atomic_set(&estate->nr_probing, alist->nr_addrs); in afs_fs_probe_fileserver()
273 afs_get_address_preferences(net, alist); in afs_fs_probe_fileserver()
276 unprobed = (1UL << alist->nr_addrs) - 1; in afs_fs_probe_fileserver()
281 for (i = 0; i < alist->nr_addrs; i++) { in afs_fs_probe_fileserver()
283 alist->addrs[i].prio > best_prio) { in afs_fs_probe_fileserver()
[all …]
A Dfs_operation.c232 struct afs_addr_list *alist; in afs_put_operation() local
256 alist = op->estate->addresses; in afs_put_operation()
257 if (alist) { in afs_put_operation()
259 op->addr_index != alist->preferred && in afs_put_operation()
260 test_bit(alist->preferred, &op->addr_tried)) in afs_put_operation()
261 WRITE_ONCE(alist->preferred, op->addr_index); in afs_put_operation()
A Drotate.c154 struct afs_addr_list *alist; in afs_select_fileserver() local
606 alist = op->estate->addresses; in afs_select_fileserver()
609 for (i = 0; i < alist->nr_addrs; i++) { in afs_select_fileserver()
612 if (alist->addrs[i].prio > best_prio) { in afs_select_fileserver()
614 best_prio = alist->addrs[i].prio; in afs_select_fileserver()
618 alist->preferred = addr_index; in afs_select_fileserver()
627 op->server_index, addr_index, alist->nr_addrs, in afs_select_fileserver()
628 rxrpc_kernel_remote_addr(alist->addrs[op->addr_index].peer)); in afs_select_fileserver()
A Dinternal.h805 struct afs_addr_list *alist; /* Current address list (pins ref) */ member
992 struct afs_addr_list *afs_get_addrlist(struct afs_addr_list *alist, enum afs_alist_trace reason);
994 extern void afs_put_addrlist(struct afs_addr_list *alist, enum afs_alist_trace reason);
1011 void afs_get_address_preferences_rcu(struct afs_net *net, struct afs_addr_list *alist);
1012 void afs_get_address_preferences(struct afs_net *net, struct afs_addr_list *alist);
1352 struct afs_addr_list *alist = op->estate->addresses; in afs_make_op_call() local
1359 call->peer = rxrpc_kernel_get_peer(alist->addrs[op->addr_index].peer); in afs_make_op_call()
1539 struct afs_addr_list *alist,
/linux/fs/xfs/
A Dxfs_handle.c360 struct xfs_attrlist *alist = context->buffer; in xfs_ioc_attr_put_listent() local
367 ASSERT(context->firstu >= sizeof(*alist)); in xfs_ioc_attr_put_listent()
376 arraytop = sizeof(*alist) + in xfs_ioc_attr_put_listent()
377 context->count * sizeof(alist->al_offset[0]); in xfs_ioc_attr_put_listent()
384 alist->al_more = 1; in xfs_ioc_attr_put_listent()
394 alist->al_count = context->count; in xfs_ioc_attr_put_listent()
432 struct xfs_attrlist *alist; in xfs_ioc_attr_list() local
475 alist = context.buffer; in xfs_ioc_attr_list()
476 alist->al_count = 0; in xfs_ioc_attr_list()
477 alist->al_more = 0; in xfs_ioc_attr_list()
[all …]
/linux/net/sched/
A Dsch_drr.c24 struct list_head alist; member
232 list_del(&cl->alist); in drr_qlen_notify()
360 list_add_tail(&cl->alist, &q->active); in drr_enqueue()
379 cl = list_first_entry(&q->active, struct drr_class, alist); in drr_dequeue()
393 list_del(&cl->alist); in drr_dequeue()
403 list_move_tail(&cl->alist, &q->active); in drr_dequeue()
434 list_del(&cl->alist); in drr_reset_qdisc()
A Dsch_ets.c40 struct list_head alist; /* In struct ets_sched.active. */ member
294 list_del(&cl->alist); in ets_class_qlen_notify()
438 list_add_tail(&cl->alist, &q->active); in ets_qdisc_enqueue()
475 cl = list_first_entry(&q->active, struct ets_class, alist); in ets_qdisc_dequeue()
489 list_del(&cl->alist); in ets_qdisc_dequeue()
494 list_move_tail(&cl->alist, &q->active); in ets_qdisc_dequeue()
652 list_add_tail(&q->classes[i].alist, &q->active); in ets_qdisc_change()
658 list_del(&q->classes[i].alist); in ets_qdisc_change()
702 INIT_LIST_HEAD(&q->classes[i].alist); in ets_qdisc_init()
714 list_del(&q->classes[band].alist); in ets_qdisc_reset()
A Dsch_qfq.c137 struct list_head alist; /* Link for active-classes list. */ member
323 list_add_tail(&cl->alist, &agg->active); in qfq_add_to_agg()
324 if (list_first_entry(&agg->active, struct qfq_class, alist) == in qfq_add_to_agg()
350 list_del(&cl->alist); /* remove from RR queue of the aggregate */ in qfq_deactivate_class()
988 list_del(&cl->alist); in agg_dequeue()
991 list_move_tail(&cl->alist, &agg->active); in agg_dequeue()
1003 *cl = list_first_entry(&agg->active, struct qfq_class, alist); in qfq_peek_skb()
1261 list_first_entry(&agg->active, struct qfq_class, alist) in qfq_enqueue()
1263 list_move_tail(&cl->alist, &agg->active); in qfq_enqueue()
1270 list_add_tail(&cl->alist, &agg->active); in qfq_enqueue()
[all …]
/linux/drivers/scsi/aic94xx/
A Daic94xx_task.c525 LIST_HEAD(alist); in asd_execute_task()
541 __list_add(&alist, ascb->list.prev, &ascb->list); in asd_execute_task()
542 list_for_each_entry(a, &alist, list) { in asd_execute_task()
547 list_for_each_entry(a, &alist, list) { in asd_execute_task()
572 list_del_init(&alist); in asd_execute_task()
577 __list_add(&alist, ascb->list.prev, &ascb->list); in asd_execute_task()
585 list_for_each_entry(a, &alist, list) { in asd_execute_task()
606 list_del_init(&alist); in asd_execute_task()
/linux/net/mptcp/
A Dpm_netlink.c1638 struct mptcp_rm_list alist = { .nr = 0 }; in mptcp_pm_remove_addrs() local
1643 if (alist.nr >= MPTCP_RM_IDS_MAX) in mptcp_pm_remove_addrs()
1653 alist.ids[alist.nr++] = entry->addr.id; in mptcp_pm_remove_addrs()
1656 if (alist.nr) { in mptcp_pm_remove_addrs()
1659 mptcp_pm_remove_addr(msk, &alist); in mptcp_pm_remove_addrs()
1668 struct mptcp_rm_list alist = { .nr = 0 }, slist = { .nr = 0 }; in mptcp_pm_flush_addrs_and_subflows() local
1676 if (alist.nr < MPTCP_RM_IDS_MAX && in mptcp_pm_flush_addrs_and_subflows()
1678 alist.ids[alist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr); in mptcp_pm_flush_addrs_and_subflows()
1682 if (alist.nr) { in mptcp_pm_flush_addrs_and_subflows()
1683 msk->pm.add_addr_signaled -= alist.nr; in mptcp_pm_flush_addrs_and_subflows()
[all …]
/linux/include/trace/events/
A Dafs.h1427 __field(unsigned int, alist)
1434 __entry->alist = alist_debug_id;
1440 __entry->alist,
1491 struct afs_addr_list *alist = estate->addresses;
1499 memcpy(&__entry->srx, rxrpc_kernel_remote_srx(alist->addrs[addr_index].peer),
1510 TP_PROTO(struct afs_vlserver *server, bool tx, struct afs_addr_list *alist,
1513 TP_ARGS(server, tx, alist, addr_index, error, abort_code, rtt_us),
1533 memcpy(&__entry->srx, rxrpc_kernel_remote_srx(alist->addrs[addr_index].peer),
/linux/Documentation/translations/zh_CN/process/
A Dcoding-style.rst607 (c-offsets-alist . (
/linux/Documentation/translations/zh_TW/process/
A Dcoding-style.rst610 (c-offsets-alist . (
/linux/Documentation/translations/it_IT/process/
A Dcoding-style.rst671 (c-offsets-alist . (
/linux/Documentation/process/
A Dcoding-style.rst667 (c-offsets-alist . (
/linux/Documentation/translations/sp_SP/process/
A Dcoding-style.rst698 (c-offsets-alist . (

Completed in 802 milliseconds