KMC 京都マイクロコンピュータ株式会社

以前にgccでNEONのSIMD命令を生成させる方法という記事を書きましたが、今はかなり状況が変わっています。コンパイラのオートベクタライズの最適化はずっと進化していて、簡単なコンパイルオプションをつけるだけでNEONのSIMD命令を活用することができるようになっています。

ビルドにmakeコマンドを使うときにはMakefileにファイルの依存関係を書いておく必要があります。

しかし、開発の途中でインクルードするヘッダファイルが増えてくると、これらの依存関係を手作業で記述するのは面倒です。(そして、これをサボったことでハマることもよくあることです。:)

ここでは、gccの機能を使ってこれを自動化する方法を紹介します。

Ubuntu 12.04LTSでのarm-linux-gnueabihf-gccのツールチェインのhfはHard Floatの意味です。

関数呼び出し規約(Calling Convention)が変更されて、double, floatの引数はFPUのレジスタに積んで渡し、戻り値もFPUのレジスタを使うようになっています。今までは、FPUが利用可能だったとしても、Soft Floatと互換性を保つために汎用レジスタで引き渡していました。当然これらは混ぜて使うことはできません。全てのライブラリに影響があります。

簡単なプログラムで実際に生成されるコードを見てみます。

SHのgccでは浮動小数点演算のオプションの指定方法が他のアーキテクチャと異なっています。

それぞれどんなコードが生成されるのか確認してみました。

昨日、自分で修正したプログラムが意図した通りに動作しなくて少し悩んだのですが、それはunsignedの型の変数に負数を代入して、0と比較している部分が正しく動かなかったためでした。unsignedの型の変数は0より小さくなることはありません。

でも、こんなケースではgccはwarningを出して教えてくれたはず。実はオプションの指定が必要でした。

NDKに含まれているgccなどのツールチェインをソースからリビルドする方法を調べました。

以前ARM11のパフォーマンスモニタを利用した簡単な実行時間の計測方法を紹介しました。今回は同じことをCortex-A9でやってみました。

先日gccの4.5.0がリリースされたので、開発用のトランクでは今は次の4.6に向けてコードのマージが行われています。

この変更点に、Android用の変更を見つけたので紹介します。

これもまた、ELC(Embedded Linux Conference)でのセッションの紹介です。

ELCのスライドのページのDenys Vlasenkoさんの"Link time dead code and data elimination using GNU toolchain"を見てください。

私がよく使うgccの便利なオプションをまたひとつ紹介します。

gccのコマンドラインオプションをちょっと調べたいときには、gcc自身のhelpが便利です。

この記事ではgcc 4.4.0を使用しています。もっと新しいgccの場合はこちら。

2013年06月27日 ARMのNEONのSIMD命令をgccのオートベクタライズの最適化で使う方法

AndroidのSDKのgoldfishのCPUをcortex-A8に置き換えてNEONのSIMD命令を試す(その2) のときにはarm_neon.hに定義されているintrinsicsを使ってNEONのSIMD命令を生成させました。この方法だとNEONの命令について詳細を知っていなければなりませんし、なによりもそのプログラムがNEONに依存したものになってしまいます。

今回はコンパイラの最適化の機能を使ってNEONのSIMD命令を生成させるコツを紹介します。

ARM11のCP15にパフォーマンスモニタがあり、そのサイクルカウンタを利用して簡単にプログラムの2点間の時間を計測することができます。

計測用の関数を手軽に使えるようにソースコードを一つのヘッダファイルにまとめてみました。

ある関数を複数の方法で実装して、どちらが速いかを比較する場合に便利です。