annotate example/word_count/gpu/Exec.cl @ 2054:2e7a6f40672f draft

add param(4) in FileMapReduce.cc
author masa
date Fri, 29 Jan 2016 15:56:28 +0900
parents 44fa0f1320a9
children
Ignore whitespace changes - Everywhere: Within whitespace: At end of lines:
rev   line source
1539
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
1 __kernel void
1836
56692133c5fb success run wordcount with gpu, but result is wrong
Shohei KOKUBO <e105744@ie.u-ryukyu.ac.jp>
parents: 1677
diff changeset
2 wordcount(__constant long *param,
56692133c5fb success run wordcount with gpu, but result is wrong
Shohei KOKUBO <e105744@ie.u-ryukyu.ac.jp>
parents: 1677
diff changeset
3 __global char *i_data,
1842
17d06be35858 fix SC failed error
yuhi
parents: 1838
diff changeset
4 __global unsigned long *o_data)
1539
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
5 {
1842
17d06be35858 fix SC failed error
yuhi
parents: 1838
diff changeset
6 __global unsigned long *head_tail_flag = o_data+2;
1836
56692133c5fb success run wordcount with gpu, but result is wrong
Shohei KOKUBO <e105744@ie.u-ryukyu.ac.jp>
parents: 1677
diff changeset
7 long length = param[0];
1838
759587e37bc7 Change to long
yuhi
parents: 1837
diff changeset
8 long word_flag = 0;
759587e37bc7 Change to long
yuhi
parents: 1837
diff changeset
9 long word_num = 0;
759587e37bc7 Change to long
yuhi
parents: 1837
diff changeset
10 long line_num = 0;
759587e37bc7 Change to long
yuhi
parents: 1837
diff changeset
11 long i = 0;
1539
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
12
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
13 head_tail_flag[0] = (i_data[0] != 0x20) && (i_data[0] != 0x0A);
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
14 word_num -= 1-head_tail_flag[0];
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
15 for (; i < length; i++) {
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
16 if (i_data[i] == 0x20) {
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
17 word_flag = 1;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
18 } else if (i_data[i] == 0x0A) {
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
19 line_num += 1;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
20 word_flag = 1;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
21 } else {
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
22 word_num += word_flag;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
23 word_flag = 0;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
24 }
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
25 }
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
26
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
27 word_num += word_flag;
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
28 head_tail_flag[1] = (i_data[i-1] != 0x20) && (i_data[i-1] != 0x0A);
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
29
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
30 // s->printf("SPE word %d line %d\n",word_num,line_num);
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
31
1842
17d06be35858 fix SC failed error
yuhi
parents: 1838
diff changeset
32 o_data[0] = (unsigned long)word_num;
17d06be35858 fix SC failed error
yuhi
parents: 1838
diff changeset
33 o_data[1] = (unsigned long)line_num;
1539
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
34
6840fa213308 recommit gputask
Yuhi TOMARI <yuhi@cr.ie.u-ryukyu.ac.jp>
parents:
diff changeset
35 }