1、  打开Eclipse,File-->New-->AndroidApplication Project-->Application Name:Hello-Neon, Project Name: Hello-Neon,Package Name:com.hello_neon.android, Minimum Required SDK:API 9:Android 2.3(Gingerbread),Next-->去掉Create custom launcher icon的勾选,Next-->Next-->ActivityName:Hello_NeonProjectActivity,Finish.

2、  打开Hello-Neon工程下的src-->com.hello_neon.android-->Hello_NeonProjectActivity.java,将其内容改为:

package com.hello_neon.android;import android.os.Bundle;
import android.app.Activity;
import android.widget.TextView;public class Hello_NeonProjectActivity extends Activity {/** Called when the activity is first created. */@Overridepublic void onCreate(Bundle savedInstanceState){super.onCreate(savedInstanceState);/* Create a TextView and set its content.* the text is retrieved by calling a native function.*/TextView  tv = new TextView(this);tv.setText( stringFromJNI() );setContentView(tv);}/* A native method that is implemented by the* 'helloneon' native library, which is packaged with this application.*/public native String  stringFromJNI();/* this is used to load the 'helloneon' library on application* startup. The library has already been unpacked into* /data/data/com.example.neon/lib/libhelloneon.so at* installation time by the package manager.*/static {System.loadLibrary("helloneon");}}

3、 保存Hello_NeonProjectActivity.java文件,打开命令行窗口,将其定位到\bin\classes目录下,输入命令:javah –classpath D:\ProgramFiles\Android\android-sdk\platforms\android-9\android.jar;com.hello_neon.android.Hello_NeonProjectActivity ,会在\bin\classes目录下生成com_hello_neon_android_Hello_NeonProjectActivity.h文件(说明:*.jar也可以是其它版本);

4、  选中Hello-Neon工程,点击右键-->New-->Folder新建一个jni文件夹,在此文件夹下添加Android.mk、Application.mk、helloneon.c、helloneon-intrinsics.c、helloneon-intrinsics.h五个文件,其中内容分别为:

Android.mk:

LOCAL_PATH := $(call my-dir)
include $(CLEAR_VARS)
LOCAL_MODULE    := helloneon#填写要编译的源文件路径
LOCAL_SRC_FILES := helloneon.c helloneon-intrinsics.c#默认包含的头文件路径
LOCAL_C_INCLUDES := \
$(LOCAL_PATH) \
$(LOCAL_PATH)/..#-g 后面的一系列项目添加了才能使用arm_neon-h头文件, -mfloat-abi=softfp -mfpu=neon 使用arm_neon.h必须
LOCAL_CFLAGS := -g -mfloat-abi=softfp -mfpu=neon -march=armv7-a -mtune=cortex-a8LOCAL_LDLIBS := -lz -llog
TARGET_ARCH_ABI := armeabi-v7a
LOCAL_ARM_MODE := armifeq ($(TARGET_ARCH_ABI),armeabi-v7a)
#采用NEON优化技术LOCAL_ARM_NEON := true#LOCAL_CFLAGS := -DHAVE_NEON=1
endifLOCAL_STATIC_LIBRARIES := cpufeatures#生成动态调用库
include $(BUILD_SHARED_LIBRARY)$(call import-module,cpufeatures)

Application.mk:

APP_PROJECT_PATH := $(call my-dir)/..
APP_PLATFORM := android-10
#choose which library to compile against in your Makefile
APP_STL := stlport_static
#APP_ABI这句指定了编译的目标平台类型,可以针对不同平台进行优化,x86 or armeabi-v7a
# Build both ARMv5TE and ARMv7-A machine code.
APP_ABI := armeabi armeabi-v7a
APP_CPPFLAGS += -fexceptions
#for using c++ features,you need to enable these in your Makefile
APP_CPP_FEATURES += exceptions rtti

helloneon.c:

#include <jni.h>
#include <time.h>
#include <stdio.h>
#include <stdlib.h>
#include <cpu-features.h>
#include "helloneon-intrinsics.h"#define DEBUG 0
#define HAVE_NEON#if DEBUG
#include <android/log.h>
#  define  D(x...)  __android_log_print(ANDROID_LOG_INFO,"helloneon",x)
#else
#  define  D(...)  do {} while (0)
#endif/* return current time in milliseconds */
static double
now_ms(void)
{struct timespec res;clock_gettime(CLOCK_REALTIME, &res);return 1000.0*res.tv_sec + (double)res.tv_nsec/1e6;
}/* this is a FIR filter implemented in C */
static void
fir_filter_c(short *output, const short* input, const short* kernel, int width, int kernelSize)
{int  offset = -kernelSize/2;int  nn;for (nn = 0; nn < width; nn++) {int sum = 0;int mm;for (mm = 0; mm < kernelSize; mm++) {sum += kernel[mm]*input[nn+offset+mm];}output[nn] = (short)((sum + 0x8000) >> 16);}
}#define  FIR_KERNEL_SIZE   32
#define  FIR_OUTPUT_SIZE   2560
#define  FIR_INPUT_SIZE    (FIR_OUTPUT_SIZE + FIR_KERNEL_SIZE)
#define  FIR_ITERATIONS    600static const short  fir_kernel[FIR_KERNEL_SIZE] = {0x10, 0x20, 0x40, 0x70, 0x8c, 0xa2, 0xce, 0xf0, 0xe9, 0xce, 0xa2, 0x8c, 070, 0x40, 0x20, 0x10,0x10, 0x20, 0x40, 0x70, 0x8c, 0xa2, 0xce, 0xf0, 0xe9, 0xce, 0xa2, 0x8c, 070, 0x40, 0x20, 0x10 };static short        fir_output[FIR_OUTPUT_SIZE];
static short        fir_input_0[FIR_INPUT_SIZE];
static const short* fir_input = fir_input_0 + (FIR_KERNEL_SIZE/2);
static short        fir_output_expected[FIR_OUTPUT_SIZE];/* This is a trivial JNI example where we use a native method* to return a new VM String. See the corresponding Java source* file located at:**   apps/samples/hello-neon/project/src/com/example/neon/HelloNeon.java*/
JNIEXPORT jstring JNICALL Java_com_hello_1neon_android_Hello_1NeonProjectActivity_stringFromJNI(JNIEnv *env, jobject thiz)
{char*  str;uint64_t features;char buffer[512];char tryNeon = 0;double  t0, t1, time_c, time_neon;/* setup FIR input - whatever */{int  nn;for (nn = 0; nn < FIR_INPUT_SIZE; nn++) {fir_input_0[nn] = (5*nn) & 255;}fir_filter_c(fir_output_expected, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}/* Benchmark small FIR filter loop - C version */t0 = now_ms();{int  count = FIR_ITERATIONS;for (; count > 0; count--) {fir_filter_c(fir_output, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}}t1 = now_ms();time_c = t1 - t0;asprintf(&str, "FIR Filter benchmark:\nC version          : %g ms\n", time_c);strlcpy(buffer, str, sizeof buffer);free(str);strlcat(buffer, "Neon version   : ", sizeof buffer);if (android_getCpuFamily() != ANDROID_CPU_FAMILY_ARM) {strlcat(buffer, "Not an ARM CPU !\n", sizeof buffer);goto EXIT;}features = android_getCpuFeatures();if ((features & ANDROID_CPU_ARM_FEATURE_ARMv7) == 0) {strlcat(buffer, "Not an ARMv7 CPU !\n", sizeof buffer);goto EXIT;}/* HAVE_NEON is defined in Android.mk ! */
#ifdef HAVE_NEONif ((features & ANDROID_CPU_ARM_FEATURE_NEON) == 0) {strlcat(buffer, "CPU doesn't support NEON !\n", sizeof buffer);goto EXIT;}/* Benchmark small FIR filter loop - Neon version */t0 = now_ms();{int  count = FIR_ITERATIONS;for (; count > 0; count--) {fir_filter_neon_intrinsics(fir_output, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}}t1 = now_ms();time_neon = t1 - t0;asprintf(&str, "%g ms (x%g faster)\n", time_neon, time_c / (time_neon < 1e-6 ? 1. : time_neon));strlcat(buffer, str, sizeof buffer);free(str);/* check the result, just in case */{int  nn, fails = 0;for (nn = 0; nn < FIR_OUTPUT_SIZE; nn++) {if (fir_output[nn] != fir_output_expected[nn]) {if (++fails < 16)D("neon[%d] = %d expected %d", nn, fir_output[nn], fir_output_expected[nn]);}}D("%d fails\n", fails);}
#else /* !HAVE_NEON */strlcat(buffer, "Program not compiled with ARMv7 support !\n", sizeof buffer);
#endif /* !HAVE_NEON */
EXIT:return (*env)->NewStringUTF(env, buffer);
}

helloneon-intrinsics.h:

#ifndef HELLONEON_INTRINSICS_H
#define HELLONEON_INTRINSICS_Hvoid fir_filter_neon_intrinsics(short *output, const short* input, const short* kernel, int width, int kernelSize);#endif /* HELLONEON_INTRINSICS_H */

helloneon-intrinsics.c:

#include "helloneon-intrinsics.h"
#include <arm_neon.h>/* this source file should only be compiled by Android.mk when targeting* the armeabi-v7a ABI, and should be built in NEON mode*/
void
fir_filter_neon_intrinsics(short *output, const short* input, const short* kernel, int width, int kernelSize)
{
#if 1int nn, offset = -kernelSize/2;for (nn = 0; nn < width; nn++){int mm, sum = 0;int32x4_t sum_vec = vdupq_n_s32(0);for(mm = 0; mm < kernelSize/4; mm++){int16x4_t  kernel_vec = vld1_s16(kernel + mm*4);int16x4_t  input_vec = vld1_s16(input + (nn+offset+mm*4));sum_vec = vmlal_s16(sum_vec, kernel_vec, input_vec);}sum += vgetq_lane_s32(sum_vec, 0);sum += vgetq_lane_s32(sum_vec, 1);sum += vgetq_lane_s32(sum_vec, 2);sum += vgetq_lane_s32(sum_vec, 3);if(kernelSize & 3){for(mm = kernelSize - (kernelSize & 3); mm < kernelSize; mm++)sum += kernel[mm] * input[nn+offset+mm];}output[nn] = (short)((sum + 0x8000) >> 16);}
#else /* for comparison purposes only */int nn, offset = -kernelSize/2;for (nn = 0; nn < width; nn++) {int sum = 0;int mm;for (mm = 0; mm < kernelSize; mm++) {sum += kernel[mm]*input[nn+offset+mm];}output[nn] = (short)((sum + 0x8000) >> 16);}
#endif
}

5、 利用NDK生成.so文件:选中工程-->Properties-->Builders-->New-->选中Program-->OK,Name:Hello_Neon_Builder,Location: D:\ProgramFiles\Android\android-sdk\android-ndk-r9\ndk-build.cmd,Working Directory: E:\NEON\Eclipse\Hello-Neon -->Apply,选中Refresh,勾选Refreshresources upon completion, 勾选Specific resources,点击Specify Resources…,勾选Hello-Neon工程下的libs文件夹,Finish-->Apply,选中BuildOptions,勾选Allocate Console(necessary for input), After a “Clean”, During manualbuilds, During auto builds, Specify working set of relevant resources,点击SpecifyResoures…,勾选Hello-Neon工程下的jni文件夹,Finish-->Apply-->OK-->OK,会在libs文件夹下生成libhelloneon.so文件;

6、  选中Hello-Neon,-->Run As-->AndroidApplication,运行结果为:

FIRFilter benchmark:

C version       :282.84 ms

Neon version    :135985 ms(x2.07994 faster)

以上是.c文件的操作步骤,若将.c文件该为.cpp文件,则需改动两个文件:

1、将Android.mk改为:

LOCAL_PATH := $(call my-dir)
include $(CLEAR_VARS)
LOCAL_MODULE    := helloneon#填写要编译的源文件路径
LOCAL_SRC_FILES := helloneon.cpp helloneon-intrinsics.cpp#默认包含的头文件路径
LOCAL_C_INCLUDES := \
$(LOCAL_PATH) \
$(LOCAL_PATH)/..#-g 后面的一系列项目添加了才能使用arm_neon-h头文件, -mfloat-abi=softfp -mfpu=neon 使用arm_neon.h必须
LOCAL_CFLAGS := -g -mfloat-abi=softfp -mfpu=neon -march=armv7-a -mtune=cortex-a8LOCAL_LDLIBS := -lz -llog
TARGET_ARCH_ABI := armeabi-v7a
LOCAL_ARM_MODE := armifeq ($(TARGET_ARCH_ABI),armeabi-v7a)
#采用NEON优化技术LOCAL_ARM_NEON := true#LOCAL_CFLAGS := -DHAVE_NEON=1
endifLOCAL_STATIC_LIBRARIES := cpufeatures#生成动态调用库
include $(BUILD_SHARED_LIBRARY)$(call import-module,cpufeatures)

2、helloneon.c改为:

#include <jni.h>
#include <time.h>
#include <stdio.h>
#include <stdlib.h>
#include <cpu-features.h>
#include "helloneon-intrinsics.h"#define DEBUG 0
#define HAVE_NEON#ifdef __cplusplus
extern "C" {
#endif#if DEBUG
#include <android/log.h>
#  define  D(x...)  __android_log_print(ANDROID_LOG_INFO,"helloneon",x)
#else
#  define  D(...)  do {} while (0)
#endif/* return current time in milliseconds */
static double
now_ms(void)
{struct timespec res;clock_gettime(CLOCK_REALTIME, &res);return 1000.0*res.tv_sec + (double)res.tv_nsec/1e6;
}/* this is a FIR filter implemented in C */
static void
fir_filter_c(short *output, const short* input, const short* kernel, int width, int kernelSize)
{int  offset = -kernelSize/2;int  nn;for (nn = 0; nn < width; nn++) {int sum = 0;int mm;for (mm = 0; mm < kernelSize; mm++) {sum += kernel[mm]*input[nn+offset+mm];}output[nn] = (short)((sum + 0x8000) >> 16);}
}#define  FIR_KERNEL_SIZE   32
#define  FIR_OUTPUT_SIZE   2560
#define  FIR_INPUT_SIZE    (FIR_OUTPUT_SIZE + FIR_KERNEL_SIZE)
#define  FIR_ITERATIONS    600static const short  fir_kernel[FIR_KERNEL_SIZE] = {0x10, 0x20, 0x40, 0x70, 0x8c, 0xa2, 0xce, 0xf0, 0xe9, 0xce, 0xa2, 0x8c, 070, 0x40, 0x20, 0x10,0x10, 0x20, 0x40, 0x70, 0x8c, 0xa2, 0xce, 0xf0, 0xe9, 0xce, 0xa2, 0x8c, 070, 0x40, 0x20, 0x10 };static short        fir_output[FIR_OUTPUT_SIZE];
static short        fir_input_0[FIR_INPUT_SIZE];
static const short* fir_input = fir_input_0 + (FIR_KERNEL_SIZE/2);
static short        fir_output_expected[FIR_OUTPUT_SIZE];/* This is a trivial JNI example where we use a native method* to return a new VM String. See the corresponding Java source* file located at:**   apps/samples/hello-neon/project/src/com/example/neon/HelloNeon.java*/
JNIEXPORT jstring JNICALL Java_com_hello_1neon_android_Hello_1NeonProjectActivity_stringFromJNI(JNIEnv *env, jobject thiz)
{char str[512] = {0};uint64_t features;char buffer[512];char tryNeon = 0;double  t0, t1, time_c, time_neon;/* setup FIR input - whatever */{int  nn;for (nn = 0; nn < FIR_INPUT_SIZE; nn++) {fir_input_0[nn] = (5*nn) & 255;}fir_filter_c(fir_output_expected, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}/* Benchmark small FIR filter loop - C version */t0 = now_ms();{int  count = FIR_ITERATIONS;for (; count > 0; count--) {fir_filter_c(fir_output, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}}t1 = now_ms();time_c = t1 - t0;sprintf(str, "FIR Filter benchmark:\nC version          : %g ms\n", time_c);strlcpy(buffer, str, sizeof buffer);strlcat(buffer, "Neon version   : ", sizeof buffer);if (android_getCpuFamily() != ANDROID_CPU_FAMILY_ARM) {strlcat(buffer, "Not an ARM CPU !\n", sizeof buffer);goto EXIT;}features = android_getCpuFeatures();if ((features & ANDROID_CPU_ARM_FEATURE_ARMv7) == 0) {strlcat(buffer, "Not an ARMv7 CPU !\n", sizeof buffer);goto EXIT;}/* HAVE_NEON is defined in Android.mk ! */
#ifdef HAVE_NEONif ((features & ANDROID_CPU_ARM_FEATURE_NEON) == 0) {strlcat(buffer, "CPU doesn't support NEON !\n", sizeof buffer);goto EXIT;}/* Benchmark small FIR filter loop - Neon version */t0 = now_ms();{int  count = FIR_ITERATIONS;for (; count > 0; count--) {fir_filter_neon_intrinsics(fir_output, fir_input, fir_kernel, FIR_OUTPUT_SIZE, FIR_KERNEL_SIZE);}}t1 = now_ms();time_neon = t1 - t0;sprintf(str, "%g ms (x%g faster)\n", time_neon, time_c / (time_neon < 1e-6 ? 1. : time_neon));strlcat(buffer, str, sizeof buffer);/* check the result, just in case */{int  nn, fails = 0;for (nn = 0; nn < FIR_OUTPUT_SIZE; nn++) {if (fir_output[nn] != fir_output_expected[nn]) {if (++fails < 16)D("neon[%d] = %d expected %d", nn, fir_output[nn], fir_output_expected[nn]);}}D("%d fails\n", fails);}
#else /* !HAVE_NEON */strlcat(buffer, "Program not compiled with ARMv7 support !\n", sizeof buffer);
#endif /* !HAVE_NEON */
EXIT:return env->NewStringUTF(buffer);
}#ifdef __cplusplus
}
#endif

参考文献:

1、  http://blog.csdn.net/fengbingchun/article/details/11580983

2、  android-ndk-r9-windows-x86_64中的hello-neon例子代码

NEON在Android中的使用举例相关推荐

  1. NEON在Android中的使用举例【转】

    转自:http://blog.csdn.net/fengbingchun/article/details/37766607 版权声明:本文为博主原创文章,未经博主允许不得转载. 1.  打开Eclip ...

  2. Android中的接口的使用举例

    这里讲解了两种大家可以在学习Android中容易对接口迷茫的两种用法 1.用于回调 我们会在子线程中执行耗时操作,就可以用接口进行耗时操作结果的回调: 首先定义一个接口 public interfac ...

  3. Android中悬浮窗口的实现原理和示例代码

    用了我一个周末的时间,个中愤懑就不说了,就这个问题,我翻遍全球网络没有一篇像样的资料,现在将实现原理简单叙述如下:调用WindowManager,并设置WindowManager.LayoutPara ...

  4. Android中的设计模式-状态模式

    原文出处:http://www.linuxidc.com/Linux/2015-04/116013.htm 状态模式说明 "状态模式允许一个对象在其内部状态改变的时候改变其行为.这个对象看上 ...

  5. Android中Canvas绘图之Shader使用图文详解

    概述 我们在用Android中的Canvas绘制各种图形时,可以通过Paint.setShader(shader)方法为画笔Paint设置shader,这样就可以绘制出多彩的图形.那么Shader是什 ...

  6. android中SELINUX规则分析和语法简介

    点击打开链接 1. SELINUX是可以理解为一种Android上面的安全机制,是有美国国家安全局和一些公司设计的一个针对linux的安全加强系统 我们可以通过配置SELINUX的相关policy,来 ...

  7. android:catation=quot;90quot;,Android中的AlarmManager的使用.htm

    var protocol = window.location.protocol; document.write(' Android中的AlarmManager的使用 - wangxingwu_314的 ...

  8. Android中使用官方提供好的功能使用说明(比如系统图库获取),也作为延生学习的学习文档

    这篇文章最核心的就是去学习如何学习Android,如何去使用Android文档. 我们一般在刚开始接触开发的时候,如果遇到无法解决的问题,常常会百度,或者google去寻找答案,比如有个需求是获取系统 ...

  9. android中获取时间

    android中获取时间 1)通过calendar类获取 Calendar calendar = Calendar.getInstance(); int moth = calendar.get(Cal ...

最新文章

  1. 企业级微服务架构统一安全认证设计与实践!
  2. Linux学习笔记——例说makefile 综合案例
  3. 关于在Intellij IDEA工具中配置热加载问题
  4. 已知项目有风险,作为项目经理接还是不接?
  5. php rss xml,php 一个完全面向对象的RSS/XML类的简单示例
  6. SGCheck:一个实验堆栈和全局数组溢出检测器
  7. 一图解析MySQL执行查询全流程
  8. windows7 x86_64系统安装xampp后apache无法启动,端口冲突
  9. cookie可存的最大限制_一文梳理Web存储,从cookie,WebStorage到IndexedDB
  10. 实战java虚拟机 百度云_《实战JAVA虚拟机 JVM故障诊断与性能优化》pdf百度云下载...
  11. 分享12306抢票心得-最终篇
  12. iOS底层探索之多线程(十八)——锁篇章的完结篇(手把手两种方式带你实现一个读写锁!)
  13. 用SQL语言操作数据
  14. mysql sql查询当天_sql查询当天数据
  15. java编写猜数字游戏_java编写猜数字游戏
  16. 【网络流量识别】【聚类】【一】模糊聚类FCS和GA—网络安全网络流量功能的模糊聚类
  17. 时分秒毫秒 正则表达式
  18. OD使用经验【转载】
  19. 计算机考研复试专业课【数据库】
  20. 大数据毕业设计选题推荐(二)

热门文章

  1. Linux那些事儿 之 戏说USB(10)模型,又见模型
  2. P2114 [NOI2014]起床困难综合症
  3. POJ1523 SPF tanjar割点求块数
  4. 计算机系统结构 网易云课堂,计算机系统结构 (三) CPU及其结构分析
  5. 【力扣网练习题】回文数
  6. 在Ubuntu 14.04 64bit上搭建Scala开发环境
  7. libcurl下载限速编程调研
  8. PHP函数printf()、sprintf()的用法
  9. 业余快速学习虚幻引擎教程
  10. Zbrush制作手榴弹案例讲解学习教程