Home
last modified time | relevance | path

Searched refs:slist (Results 1 – 25 of 29) sorted by relevance

12

/linux/tools/perf/util/
H A Dstrlist.c57 int strlist__add(struct strlist *slist, const char *new_entry) in strlist__add() argument
59 return rblist__add_node(&slist->rblist, new_entry); in strlist__add()
62 int strlist__load(struct strlist *slist, const char *filename) in strlist__load() argument
78 err = strlist__add(slist, entry); in strlist__load()
89 void strlist__remove(struct strlist *slist, struct str_node *snode) in strlist__remove() argument
91 rblist__remove_node(&slist->rblist, &snode->rb_node); in strlist__remove()
94 struct str_node *strlist__find(struct strlist *slist, const char *entry) in strlist__find() argument
97 struct rb_node *rb_node = rblist__find(&slist->rblist, entry); in strlist__find()
105 static int strlist__parse_list_entry(struct strlist *slist, const char *s, in strlist__parse_list_entry() argument
112 return strlist__load(slist, s + 7); in strlist__parse_list_entry()
[all …]
H A Dstrlist.h30 struct strlist *strlist__new(const char *slist, const struct strlist_config *config);
31 void strlist__delete(struct strlist *slist);
33 void strlist__remove(struct strlist *slist, struct str_node *sn);
34 int strlist__load(struct strlist *slist, const char *filename);
35 int strlist__add(struct strlist *slist, const char *str);
37 struct str_node *strlist__entry(const struct strlist *slist, unsigned int idx);
38 struct str_node *strlist__find(struct strlist *slist, const char *entry);
40 static inline bool strlist__has_entry(struct strlist *slist, const char *entry) in strlist__has_entry() argument
42 return strlist__find(slist, entry) != NULL; in strlist__has_entry()
45 static inline bool strlist__empty(const struct strlist *slist) in strlist__empty() argument
[all …]
H A Dthread_map.c168 struct strlist *slist = strlist__new(pid_str, NULL); in thread_map__new_by_pid_str() local
170 if (!slist) in thread_map__new_by_pid_str()
173 strlist__for_each_entry(pos, slist) { in thread_map__new_by_pid_str()
203 strlist__delete(slist); in thread_map__new_by_pid_str()
224 struct strlist *slist; in thread_map__new_by_tid_str() local
230 slist = strlist__new(tid_str, NULL); in thread_map__new_by_tid_str()
231 if (!slist) in thread_map__new_by_tid_str()
234 strlist__for_each_entry(pos, slist) { in thread_map__new_by_tid_str()
254 strlist__delete(slist); in thread_map__new_by_tid_str()
H A Dintlist.c114 struct intlist *intlist__new(const char *slist) in intlist__new() argument
124 if (slist && intlist__parse_list(ilist, slist)) in intlist__new()
H A Dintlist.h20 struct intlist *intlist__new(const char *slist);
/linux/fs/afs/
H A Dserver_list.c12 void afs_put_serverlist(struct afs_net *net, struct afs_server_list *slist) in afs_put_serverlist() argument
16 if (slist && refcount_dec_and_test(&slist->usage)) { in afs_put_serverlist()
17 for (i = 0; i < slist->nr_servers; i++) in afs_put_serverlist()
18 afs_unuse_server(net, slist->servers[i].server, in afs_put_serverlist()
20 kfree_rcu(slist, rcu); in afs_put_serverlist()
31 struct afs_server_list *slist; in afs_alloc_server_list() local
54 slist = kzalloc_flex(*slist, servers, nr_servers); in afs_alloc_server_list()
55 if (!slist) in afs_alloc_server_list()
60 slist->ro_replicating = AFS_RO_REPLICATING_USE_OLD; in afs_alloc_server_list()
62 slist->ro_replicating = AFS_RO_REPLICATING_USE_NEW; in afs_alloc_server_list()
[all …]
H A Dvolume.c80 struct afs_server_list *slist; in afs_alloc_volume() local
112 slist = afs_alloc_server_list(volume, params->key, vldb); in afs_alloc_volume()
113 if (IS_ERR(slist)) { in afs_alloc_volume()
114 ret = PTR_ERR(slist); in afs_alloc_volume()
118 *_slist = slist; in afs_alloc_volume()
119 rcu_assign_pointer(volume->servers, slist); in afs_alloc_volume()
136 struct afs_server_list *slist; in afs_lookup_volume() local
139 candidate = afs_alloc_volume(params, vldb, &slist); in afs_lookup_volume()
145 afs_attach_volume_to_servers(volume, slist); in afs_lookup_volume()
240 struct afs_server_list *slist = rcu_access_pointer(volume->servers); in afs_destroy_volume() local
[all …]
H A Dvalidation.c156 const struct afs_server_list *slist; in __afs_is_server_excluded() local
162 slist = rcu_dereference(volume->servers); in __afs_is_server_excluded()
163 for (i = 0; i < slist->nr_servers; i++) { in __afs_is_server_excluded()
164 se = &slist->servers[i]; in __afs_is_server_excluded()
330 struct afs_server_list *slist = op->server_list; in afs_update_volume_state() local
331 struct afs_server_entry *se = &slist->servers[op->server_index]; in afs_update_volume_state()
H A Dfs_probe.c317 struct afs_server_list *slist = op->server_list; in afs_wait_for_fs_probes() local
321 _enter("%u", slist->nr_servers); in afs_wait_for_fs_probes()
323 for (i = 0; i < slist->nr_servers; i++) { in afs_wait_for_fs_probes()
335 for (i = 0; i < slist->nr_servers; i++) in afs_wait_for_fs_probes()
336 add_wait_queue(&slist->servers[i].server->probe_wq, &states[i].probe_waiter); in afs_wait_for_fs_probes()
342 for (i = 0; i < slist->nr_servers; i++) { in afs_wait_for_fs_probes()
364 for (i = 0; i < slist->nr_servers; i++) in afs_wait_for_fs_probes()
365 remove_wait_queue(&slist->servers[i].server->probe_wq, &states[i].probe_waiter); in afs_wait_for_fs_probes()
H A Dcallback.c162 struct afs_server_list *slist = rcu_dereference(volume->servers); in afs_break_volume_callback() local
167 for (i = 0; i < slist->nr_servers; i++) in afs_break_volume_callback()
168 if (slist->servers[i].server == server) in afs_break_volume_callback()
169 slist->servers[i].cb_expires_at = AFS_NO_CB_PROMISE; in afs_break_volume_callback()
H A Dinternal.h1581 static inline struct afs_server_list *afs_get_serverlist(struct afs_server_list *slist) in afs_get_serverlist() argument
1583 refcount_inc(&slist->usage); in afs_get_serverlist()
1584 return slist; in afs_get_serverlist()
1592 void afs_attach_volume_to_servers(struct afs_volume *volume, struct afs_server_list *slist);
1593 void afs_reattach_volume_to_servers(struct afs_volume *volume, struct afs_server_list *slist,
1595 void afs_detach_volume_from_servers(struct afs_volume *volume, struct afs_server_list *slist);
H A Ddir.c744 struct afs_server_list *slist; in afs_server_supports_ibulk() local
754 slist = rcu_dereference(volume->servers); in afs_server_supports_ibulk()
756 for (i = 0; i < slist->nr_servers; i++) { in afs_server_supports_ibulk()
757 server = slist->servers[i].server; in afs_server_supports_ibulk()
/linux/drivers/media/common/saa7146/
H A Dsaa7146_core.c175 if (!(pt->slist = vmalloc_to_sg(mem, pages))) in saa7146_vmalloc_build_pgtable()
182 slen = dma_map_sg(&pci->dev, pt->slist, pt->nents, DMA_FROM_DEVICE); in saa7146_vmalloc_build_pgtable()
186 if (0 != saa7146_pgtable_build_single(pci, pt, pt->slist, slen)) in saa7146_vmalloc_build_pgtable()
192 dma_unmap_sg(&pci->dev, pt->slist, pt->nents, DMA_FROM_DEVICE); in saa7146_vmalloc_build_pgtable()
196 kfree(pt->slist); in saa7146_vmalloc_build_pgtable()
197 pt->slist = NULL; in saa7146_vmalloc_build_pgtable()
206 dma_unmap_sg(&pci->dev, pt->slist, pt->nents, DMA_FROM_DEVICE); in saa7146_vfree_destroy_pgtable()
208 kfree(pt->slist); in saa7146_vfree_destroy_pgtable()
209 pt->slist = NULL; in saa7146_vfree_destroy_pgtable()
/linux/drivers/net/wireless/ath/ath12k/
H A Ddp.c551 struct hal_wbm_idle_scatter_list *slist = dp->scatter_list; in ath12k_dp_scatter_idle_link_desc_cleanup() local
555 if (!slist[i].vaddr) in ath12k_dp_scatter_idle_link_desc_cleanup()
559 slist[i].vaddr, slist[i].paddr); in ath12k_dp_scatter_idle_link_desc_cleanup()
560 slist[i].vaddr = NULL; in ath12k_dp_scatter_idle_link_desc_cleanup()
572 struct hal_wbm_idle_scatter_list *slist = dp->scatter_list; in ath12k_dp_scatter_idle_link_desc_setup() local
592 slist[i].vaddr = dma_alloc_coherent(ab->dev, in ath12k_dp_scatter_idle_link_desc_setup()
594 &slist[i].paddr, GFP_KERNEL); in ath12k_dp_scatter_idle_link_desc_setup()
595 if (!slist[i].vaddr) { in ath12k_dp_scatter_idle_link_desc_setup()
602 scatter_buf = slist[scatter_idx].vaddr; in ath12k_dp_scatter_idle_link_desc_setup()
625 scatter_buf = slist[scatter_idx].vaddr; in ath12k_dp_scatter_idle_link_desc_setup()
[all …]
/linux/drivers/w1/
H A Dw1_int.c54 INIT_LIST_HEAD(&dev->slist); in w1_alloc_dev()
183 list_for_each_entry_safe(sl, sln, &dev->slist, w1_slave_entry) { in __w1_remove_master_device()
H A Dw1.c368 list_for_each_safe(ent, n, &md->slist) { in w1_master_attribute_show_slaves()
437 list_for_each_entry(sl, &dev->slist, w1_slave_entry) { in w1_slave_search_device()
705 list_add_tail(&sl->w1_slave_entry, &sl->master->slist); in __w1_attach_slave_device()
845 list_for_each_entry(iter, &dev->slist, w1_slave_entry) { in w1_search_slave()
876 list_for_each_entry_safe(sl, sln, &dev->slist, w1_slave_entry) { in w1_reconnect_slaves()
1090 list_for_each_entry(sl, &dev->slist, w1_slave_entry) in w1_search_process_cb()
1097 list_for_each_entry_safe(sl, sln, &dev->slist, w1_slave_entry) { in w1_search_process_cb()
/linux/drivers/hid/amd-sfh-hid/sfh1_1/
H A Damd_sfh_init.c20 struct sfh_sensor_list *slist; in amd_sfh_get_sensor_num() local
26 slist = &binfo.sbase.s_list; in amd_sfh_get_sensor_num()
36 if (BIT(i) & slist->sl.sensors) in amd_sfh_get_sensor_num()
/linux/fs/9p/
H A Dv9fs.c514 list_add(&v9ses->slist, &v9fs_sessionlist); in v9fs_session_init()
551 list_del(&v9ses->slist); in v9fs_session_close()
595 list_for_each_entry(v9ses, &v9fs_sessionlist, slist) { in caches_show()
H A Dv9fs.h131 struct list_head slist; /* list of sessions registered with v9fs */ member
/linux/net/mptcp/
H A Dpm_kernel.c1228 struct mptcp_rm_list alist = { .nr = 0 }, slist = { .nr = 0 }; in mptcp_pm_flush_addrs_and_subflows() local
1232 if (slist.nr < MPTCP_RM_IDS_MAX && in mptcp_pm_flush_addrs_and_subflows()
1234 slist.ids[slist.nr++] = mptcp_endp_get_local_id(msk, &entry->addr); in mptcp_pm_flush_addrs_and_subflows()
1246 if (slist.nr) in mptcp_pm_flush_addrs_and_subflows()
1247 mptcp_pm_rm_subflow(msk, &slist); in mptcp_pm_flush_addrs_and_subflows()
/linux/include/linux/
H A Dw1.h210 struct list_head slist; member
/linux/sound/soc/intel/avs/
H A Dpath.c176 unsigned int *rlist, *clist, *slist; in avs_path_set_constraint() local
185 slist = kcalloc(i, sizeof(*slist), GFP_KERNEL); in avs_path_set_constraint()
186 if (!rlist || !clist || !slist) in avs_path_set_constraint()
221 slist[i] = path_template->fe_fmt->bit_depth; in avs_path_set_constraint()
233 sample_bits_list->list = slist; in avs_path_set_constraint()
237 kfree(slist); in avs_path_set_constraint()
/linux/drivers/media/dvb-frontends/
H A Ddib8000.c2518 u8 slist = 0; in dib8000_autosearch_start() local
2571 slist = 16; in dib8000_autosearch_start()
2574 dib8000_set_isdbt_common_channel(state, slist, 1); in dib8000_autosearch_start()
2611 slist = 7; in dib8000_autosearch_start()
2618 slist = 7; in dib8000_autosearch_start()
2622 slist = 3; in dib8000_autosearch_start()
2627 slist = 2; in dib8000_autosearch_start()
2630 slist = 0; in dib8000_autosearch_start()
2633 dprintk("Using list for autosearch : %d\n", slist); in dib8000_autosearch_start()
2635 dib8000_set_isdbt_common_channel(state, slist, 1); in dib8000_autosearch_start()
/linux/drivers/w1/slaves/
H A Dw1_therm.c1498 list_for_each_entry(sl, &dev_master->slist, w1_slave_entry) { in trigger_bulk_read()
1538 &dev_master->slist, w1_slave_entry) { in trigger_bulk_read()
1567 list_for_each_entry(sl, &dev_master->slist, w1_slave_entry) { in trigger_bulk_read()
1935 list_for_each_entry(sl, &dev_master->slist, w1_slave_entry) { in therm_bulk_read_show()
/linux/include/media/drv-intf/
H A Dsaa7146.h71 struct scatterlist *slist; member

12