パスワードを忘れた? アカウント作成

tamanegiさんのトモダチの日記みんなの日記も見てね。 過去1週間(やそれより前)のストーリは、ストーリアーカイブで確認できますよ。

13224417 journal
日記

tamanegiの日記: cudaメモ

日記 by tamanegi

同一 warp 内のスレッドは __syncthreads で同期する必要はないけど、同一 warp 内での shared や global メモリへの書き込みを __threadfence(_block) とかで同期する必要がある場合は存在する。自分で書いたものは良いみたいなんだけど、他人が書いたものはそういうわけにはいかないらしい。たとえ同じ warp 内であっても。

# これになかなか気づけなくて今日は半日無駄にしたorz
# そしてやっと動いたコードのパフォーマンスがイマイチであることも発覚した
# かなしい…

13097511 journal
日記

tamanegiの日記: 【備忘録】CUDAその5

日記 by tamanegi

その1 https://srad.jp/~tamanegi/journal/605068/
その2 https://srad.jp/~tamanegi/journal/607434/
その3 https://srad.jp/~tamanegi/journal/607985/
その4 https://srad.jp/~tamanegi/journal/608006/

他の問題箇所を修正したりちょっとしたチューニング(ありがとうnvvp)

ちょっと正確な速度を知りたくなった

ためしにunique_copyの箇所をGPU(thrust)にやらせてみる

アレ?動くじゃん

(゚д゚)ウマー?

ただし、デバッグ用なオプション(-g -G -lineinfo)をつけると今でもダメらしい。まぁ、-Gをつけると何かあるんだろう。エラーメッセージもmisalignedで前と同じ。非デバッグ時の出力はcpu側でstlにやらせたのと同じだったので、正常に動作してるっぽい。ところで前回はコンパイルオプションによらずに死んでたって自分が書いてるんだけど…気のせいだったのか?最近なんか忙しすぎたり体調良くなかったりするせいか色々思い出せない……コード戻して試し直すのはめんどくさいなぁ。あんま意味無いし。

# なお、切り出したコードについてはデバッグ用オプション
# つけてもつけなくても問題無かった。

13044315 journal
日記

tamanegiの日記: 【作業ログ】DHCPサーバが動かない【解決】 8

日記 by tamanegi

12/12 19:00追記: 解決しました。ACのコメント通り、Win側がおかしかったみたいです。こっちは正直全然疑ってなかった…つまりは以下の作業のすべては割と無意味だったw

@Debian testing(stretch)

症状:
WindowsからLinux鯖にDHCPでアドレスもらおうとしたらもらえなかった。先週末あたりに鯖のアップデートをしたのが原因な気がする。

作業ログ(備忘録):
-いくつか試してみたけど全くわからない。ログを見ても怪しい点は無い
-lennyのころからつぎたして(?)使ってきたシステムなのでそろそろヤバい?
-(HWは何度か更新されてるけどクリーンインストールは全くやってなかった)
-i686からamd64に移行。自分のホームディレクトリはキープ
-pppの設定でちょっと苦戦したけどなんとか設定完了
-その他諸々適当に設定。ついでに日本語環境をfcitxに移行
-案の定DHCPサーバ(isc-dhcp-server)は起動はするがアドレス配布できない
-dnsmasqやkea-dhcp4-serverを試してみる
-起動はするが、やっぱりアドレスは割り当てられない
-エラーは特に出ないので割と途方に暮れる
-この辺りでだいぶ焦ってくる
-Win側に手動でIPを割り当ててみる
-正常に動作。まさに完璧。forwarding, natも問題なし。
-Winの設定を元に戻して、鯖でtcpdumpしてパケット見る
-netbios-nsとかのが飛んできてる
-DHCP鯖でnetbiosとかの設定を足してみるがやっぱりダメ
-iptablesとかの設定で何かしてるのかと思って外してみたけど変化なし
-あまりに眠いので敗走

misc:
-DHCPサーバそのもの(isc,dnsmasq,kea)の問題じゃない気がする
-network-managerあたりを疑うべき?kernelは…ないよね?
-どうでもいいけど、keaの設定ファイルは人間には書きにくい
-systemdのおかげかネットワークまわりの仕様がちょっと変わってるからこの辺怪しい?
-(tcpdump動かせたし、natもできたから大丈夫だと思うけど…)
-Win側はあんまり原因ぽくない。別に一台あったので試したけど症状一緒だった

13000037 journal
日記

tamanegiの日記: [備忘録] CUDA その4

日記 by tamanegi

その1 https://srad.jp/~tamanegi/journal/605068/
その2 https://srad.jp/~tamanegi/journal/607434/
その3 https://srad.jp/~tamanegi/journal/607985/

結局今日試すことにした。
unique_copyだけをとりあえずcpu側でやってみたら正常に動いた。
実行速度にそこまで影響するわけでもないからとりあえずこれで。
結局原因はわからない。切り出した場合は正常に動作するし…
thrustの中身を見る時間や元気は無い。

とりあえず投了。一応ログだけ残す。(CUDA 8, thrust 1.8.3)
- コンパイルオプションはいくつか試したけど影響なし
- 該当箇所を切り出した場合は正常に動作した
- 切り出してrdc使った場合も普通に動いた
- stable_sortは問題なかった
- Fermiでは何をしても動いた(これだけ CUDA 7.5 で検証)
- 二ヶ所使ってたunique_copyはどっちも死んでた

ホントはrdc外して検証したいとこなんだけど、大工事なので…
あ、Keplerでエラーが違ってたのは簡単に検証してもいいかも。

つか、やっと動いたけどおっせぇな、このコード。
いくらチューニングほとんどしてないとはいえ。
早めに最低限のチューニングはしておかないと。

12999350 journal
日記

tamanegiの日記: [備忘録] CUDA その3

日記 by tamanegi

その1 https://srad.jp/~tamanegi/journal/605068/
その2 https://srad.jp/~tamanegi/journal/607434/

やっとCUDA 8, thrust 1.8.3でテストできた。
んで結論、動きませんでしたw わけわからんwww
もはやFermiで動くのがおかしいんじゃないかと思い始めてきた。

とりあえずthrustのルーチン内で死ぬ。misalignedとか言われる。
今回はきちんと確認してないけど、unique_copyのトコロと推定。
これでstable_sortの方だったらやだなw

# なお、memcheckしない場合は別の場所で死ぬ。
# この辺の状態は 8.0 RC の時と同じ。

* 取扱い中のデータはおかしくないはず
* 切り出すと再現しない

とりあえず対策(というか検証方法)は

* unique_copyを自前に。それくらいなら簡単に書ける(ただし効率はお察し)
* きっと問題はrdcにあると信じてrdcを外す
* 他

とりあえず一番目を試して動いたら……って、これで動いても意味わからん
のだよなぁ。せめて自分で書いたものも落ちてくれればもうちょっとなんとか
なる気もする。何となくそうはならない気がするけど。

以上とは別に、今回CUDA 8にしてcuda-memcheckにかけたら今まで気づいて
いなかったエラーが発見できた。上の問題の原因ではなかったけど…

週明けくらいに一気に調べてみるか。一応それくらいの時間はありそうだ。

12976133 journal
日記

tamanegiの日記: [備忘録] CUDA, Thrust続き

日記 by tamanegi

いまだにCUDA 8は試せてないけど、CUDA 8 RCの段階では thrust::unique_copy がなぜか死ぬ@GTX1080。なお、やっぱりFermiでは正常に動作した。(Keplerは今回試してない。空きがなかったので…)エラー時はmisalignedとかで怒られる。つかstable_sortで死んでるんだと思ってたが違ってた。

今回は問題になってるところだけを切り出した(rdc無し; 単一ファイル)んだけど、普通に動いた。まぁここまでは一応予想していた。んで、無理矢理rdc使ってビルドすれば死ぬと予想してたんだけど、そういうわけでもなかった。疑ってごめん。本格的な調査はCUDA 8正式版(thrustのバージョンも変わる?)を試せる状況になってからだけど、直ってるといいなぁ。思った以上にめんどい。

ToDo:
*CUDA 8正式版でチェック
*Keplerでもチェック
*エラーになる条件を探す(CUDA 8でもダメな場合)

12871940 journal
日記

tamanegiの日記: メモ: CUDA

日記 by tamanegi

休み中に忘れそうなので今のうちにメモ

症状:
Fermiでは正常に動くが、KeplerやPascalでは死ぬ。KeplerとPascalで死ぬ場所はだいぶ違う。ていうか挙動そのものが大きく違う気がする。Keplerについてはコードのはじめのほうで呼ばれるcudaStreamCreateで20分くらい固まるwwまじイミフ。

原因 & 対策:
不明 & わけわかめ。ただし、
http://stackoverflow.com/questions/37526858/cuda-rdc-thrust-in-multiple-shared-objects-results-in-sigsev-in-registerentr
が関係あるかも。cc3.5 で thrust と rdc 使うあたりはほぼ共通。とりあえず様子見か。コード公開できないから、休みあけにでもテスト用コード作った方がいいかも。thrustやめるのはちょっときついからなぁ。どうしよう。つかこれNの方で直したとしても自分の手元におりてくるまでにだいぶかかりそうな気がする。

thrustのsort, uniqueだけ使っていた時はrdcやっても問題なかった気がする。cudaStreamCreateが20分固まることもなかった。1-2分は固まってた気もするが。device_vectorでのアロケーションやめればなんとかなるんかな?いや、それもだいぶめんどいな。……がんばれ休み後の自分…

12804764 journal
日記

tamanegiの日記: くだ 1

日記 by tamanegi

指定したshared memoryのサイズが大きかったのは確かに自分が悪い
しかし-Gとか-gとか付けてコンパイルして、cuda-memcheck使って実行したのに
エラーも何も書かず、落ちたりもせず、カーネルの実行を華麗にスルーするのは
どうかと思う。

詳細なエラーはなくてもいいけど、せめて次のsyncあたりで死んで欲しかった…

# nvcc や cuda-memcheck に何か他のオプション渡せば教えてくれたのかなぁ

12686649 journal
日記

tamanegiの日記: 3D麻雀

日記 by tamanegi

新しいケータイでぼんやりアプリリスト見てたらあったので入れてみた
息抜きのためにいれたんだけど割と手強いのであまり息抜きにならないw
てゆーか場合によってはストレスたまる

# 最近のケータイアプリ多すぎてわけわからんなぁ

typodupeerror

「毎々お世話になっております。仕様書を頂きたく。」「拝承」 -- ある会社の日常

読み込み中...