カテゴリ:PCとか( 99 )

もくじ

V-scale というオープンソースマイコンを拾ってきて FPGA に乗せて遊んでます

_コンソール付きのシミュレータが欲しい 端末 XMODEM
乗算・除算器を改良した話 : github
FPU 拡張を追加したい話
_演算器のモデル記述 FADD FMUL FMADD FDIV FSQRT : github
_組み込み 転送 演算器

[PR]
by tom01h | 2017-12-31 23:59 | PCとか | Trackback | Comments(0)

Verilator を OpenMP で高速化

Varilator はせっかく高速なシミュレータなのに、シングルスレッドでしか動作しない。どうせテストベンチはC++なのだから、今どきの並列化手法が使えるのじゃないか?ちょっと調べてみると、MPIのほうが高速になるらしいけど、OpenMPのほうが簡単(変更量が少ない)そうなので、こっちを使うことにした。期待はずれかもしれませんが、回路の分割じゃなくて、テストベクタの分割ですよ。それならタスクで分割すればいいじゃんて言われたらごもっとも。
まずは適当にググって最外ループを並列化してみた。軒並みフェイルしますよ。どうやら、並列化するループ内の変数を、private宣言しなくてはならないらしい。Verilatorで言うと、並列化する分だけ対象回路をインスタンスするって事か?まぁ、当然のような気もするが、なんかもったいないよね。なので、最外ループを分割してみました。
やりかたを大雑把に。元のテストベンチがこんな感じなら
Vhoge* verilator_top = new Vhoge;
for(i=0; i<100; i++){
verilator_top->in=i;
verilator_top->eva l();
if(verilator_top->out != hoge){
printf("NG\n");
}
}
delete verilator_top;
こんな風にします
Vhoge* verilator_top;
#ifdef _OPENMP
#pragma omp parallel for private(i,verilator_top)
#endif
for(t=0; t<10; t++){
verilator_top = new Vhoge;
for(i=t*10; i<(t+1)*10; i++){
verilator_top->in=i;
verilator_top->eva l();
if(verilator_top->out != hoge){
printf("NG\n");
}
}
delete verilator_top;
}

Verilator のオプションに以下を追加します。
--CFLAGS -fopenmp
--LDFLAGS -fopenmp
さらにループがネストしたりしていたら、例えばjもprivate宣言に追加します。
これでとりあえずパスはするようになったし、高速化もできました。もともと4コア8スレッドで17-8%のCPU使用率が100%になって、4-5倍ほど高速化してます。単純な回路の網羅的検証には有効なようです。ただし、ちゃんと検証できているかの確認は簡単にしかしていません。

[PR]
by tom01h | 2017-05-23 20:45 | PCとか | Trackback | Comments(0)

Verilator と OpenMP

Verilator の特徴を考えると、演算器とかの単純な回路の網羅検証が向いているのかと勝手に決めつけています。がしかし、シミュレータはシングルスレッドで動くのですよね。もったいないので、OpenMP を使った並列化の方法を考え中。
誰かいい方法知ってたら教えて下さい。うまくできたらまた報告します。

[PR]
by tom01h | 2017-05-22 20:52 | PCとか | Trackback | Comments(0)

Insider Preview 16184

ネットワークドライブがマウントできるようになったとの事で、Inspiron でもう一度 Insider Preview を使うことにしました。まず Fast で登録して、すぐに Slow に切り替えました。また何か使いたい機能があった時に Fast にするかもしれませんが…


[PR]
by tom01h | 2017-05-02 22:22 | PCとか | Trackback | Comments(0)

Petalinux for Arty Z7

Petalinux とやらをブートしてみる。これに従って pre-build を試しただけですが…
ちなみに、ちょうど良い MicroSD を持っていなかったので、小さい USB メモリを破壊して取り出しました。噂通りに MicroSD と下の基盤が入っていました。
f0054075_14534190.png

[PR]
by tom01h | 2017-05-01 18:21 | PCとか | Trackback | Comments(0)

モバイルモニター

ドスパラのモバイルモニターを買いました。タブレットの画面だけを切り売りしている感じの物です。なんか発色が悪いですねぇ。音もいかにもモバイルって感じです。
別に外でデモをしようなんて事はないと思うんですけどね。無くなる前に買っておきました。
f0054075_22512771.jpg

[PR]
by tom01h | 2017-04-30 22:54 | PCとか | Trackback | Comments(0)

Insider Preview 16176

Creators Update に合わせて Insider Preview を使うのはやめていたのですが、うれしい事にまた使う理由ができたみたいです。ファイルシステムが強化されて、ネットワークドライブがマウントできるようになったみたいです。Inspiron はもう一度 Insider Preview にするか。
[PR]
by tom01h | 2017-04-28 21:49 | PCとか | Trackback | Comments(0)

Arty Z7-20 Hdmi Out

Arty Z7 の HDMI 出力サンプルを試してみたいと思います。説明は ここ にあります。
まずは ここ からソースを取ってきます。TMDS がどうのこうの言ってコンパイルが通りません。ブロックダイアルラムを見ると、RGB to DVI Video Encoder なるモジュールの出力が浮いています。
このままでは良く分からないので、今度は ここ からとってきます。なぜか同じようなものが2個あるのですが、こっちは Xilinx のモジュールを TCL スクリプトから生成する(取って来るだけ?)、前の奴はすでに生成済みのを使う違いがあるみたいです。
f0054075_22234112.jpg
ブロックダイアグラムはこんな感じ。小さくて見えないでしょうが、右上にあるのが問題の TMDS 端子のようです。ちゃんと繋がっています。
f0054075_22274295.png
これに対して TMDS の繋がっていない方はこんな感じです。何が悪くて切れちゃっているのかは解析できず…
f0054075_22325894.png

[PR]
by tom01h | 2017-04-23 23:19 | PCとか | Trackback | Comments(0)

ARTY Z7 買った

当然ながら、欲しいのを我慢することはできません。欲しかったので買いました。使い方はこれから考えます。買うばっかじゃなく、ちゃんと使えよって話もありますが…
ARTY Z7 はちょっと長いかと思っていたのですが、 ARTY と同じ大きさでした。そして相変わらず小さな箱に、ボードが1枚だけ入っています。マイクロSDもついてません。ケーブルもなければ説明書もない。ネットを使えない人を切り捨てていく姿勢は素晴らしいと思います。
ちゃんと 20 が届きましたよ。
f0054075_22404855.jpgf0054075_22404944.jpg
[PR]
by tom01h | 2017-04-18 22:42 | PCとか | Trackback | Comments(0)

ARTY Z7

秋月電子で ARTY Z7扱いが始まった みたいです。
Zynq って言う、ARM をハードマクロで混載した FPGA を乗っけています。これがあれば、理屈的には Rocket-chip で Linux を動かしたりできるはず。まぁ、変更なしで動く環境は配ってないけど。
これあると、何か新しい遊びできるかな?とりあえず買ってみるか?その前に、V-scale chip 直せって言われそうですが…

[PR]
by tom01h | 2017-04-16 23:39 | PCとか | Trackback | Comments(0)