• <tr id="yyy80"></tr>
  • <sup id="yyy80"></sup>
  • <tfoot id="yyy80"><noscript id="yyy80"></noscript></tfoot>
  • 99热精品在线国产_美女午夜性视频免费_国产精品国产高清国产av_av欧美777_自拍偷自拍亚洲精品老妇_亚洲熟女精品中文字幕_www日本黄色视频网_国产精品野战在线观看 ?

    基于申威眾核處理器的Office口令恢復(fù)技術(shù)

    2021-06-03 06:39:16董本松趙榮彩
    計算機技術(shù)與發(fā)展 2021年5期
    關(guān)鍵詞:口令處理器運算

    董本松,趙榮彩,張 恒

    (1.中原工學(xué)院 計算機學(xué)院,河南 鄭州 450007;2.中原工學(xué)院 前沿信息技術(shù)研究院,河南 鄭州 450007)

    0 引 言

    當(dāng)前,很多數(shù)據(jù)的存儲和傳輸都經(jīng)過各種方式加密[1],使數(shù)據(jù)更加安全。但是,加密口令一旦丟失,將給用戶帶來巨大的損失;與此同時,敵對分子也會利用各種加密手段,隱藏不法行為信息,給安全部門及時獲取有效情報帶來了挑戰(zhàn)。隨著加密算法的進步以及密鑰位數(shù)的不斷增加,口令恢復(fù)的計算規(guī)模呈指數(shù)級增長[2]。針對大規(guī)模計算問題,需要一種新型的高性能口令恢復(fù)方案,以實現(xiàn)大規(guī)模計算資源的動態(tài)聚合,進而實現(xiàn)對密數(shù)據(jù)的高效分析與恢復(fù)。

    國內(nèi)外許多學(xué)者對Office口令恢復(fù)進行了大量的研究,開發(fā)了許多實用的恢復(fù)工具。AOPR(advanced office password recovery)單機版是一款專業(yè)的Office口令恢復(fù)工具,在口令恢復(fù)過程中使用CPU,但不支持GPU加速。EDPR(Elcomsoft distributed password recovery)是一款商用的口令恢復(fù)工具,支持GPU加速,但是具有平臺局限性,僅能恢復(fù)Windows上的軟件程序和文件。另外,從經(jīng)濟成本的角度來看,該軟件完成一次恢復(fù)代價較高。Hashcat自稱是世界速度最快、完全免費且開源的分布式口令恢復(fù)工具,但并不支持在SW26010眾核處理器上部署。如文獻[3-9]所示,盡管學(xué)者們對Office口令恢復(fù)做了大量的研究工作,但是口令恢復(fù)在吞吐量、效率、開銷和速度方面仍有改進的空間。

    為了解決口令恢復(fù)的大規(guī)模計算問題,該文提出了基于申威眾核處理器的Office口令恢復(fù)優(yōu)化方法。通過實驗對該方法的正確性、有效性進行了分析和驗證。實驗結(jié)果表明,該方法具有并行性強、恢復(fù)速度快、吞吐量大等特點。從個人安全層面來看,有效解決了因遺忘口令造成重要數(shù)據(jù)丟失的問題。從國家安全層面上來看,可以幫助安全部門從大規(guī)模數(shù)據(jù)中迅速獲取有效信息,對危害民族團結(jié)和國家安全的行為進行嚴厲打擊。

    該文完成了以下工作:

    (1)基于申威眾核處理器的一個主核,對Office口令恢復(fù)程序進行了一系列的分析和測試,找出了Office口令恢復(fù)程序的性能瓶頸;

    (2)結(jié)合申威眾核處理器的特點,提出了三種Office口令恢復(fù)并行機制。如加速循環(huán)并行化、優(yōu)化全局訪存操作、提高數(shù)據(jù)傳輸效率;

    (3)實現(xiàn)了申威眾核處理器的并行SW-Office口令恢復(fù)并進行了全面評估。實驗結(jié)果表明,基于申威眾核處理器的Office口令恢復(fù)程序具有良好的加速比。

    1 相關(guān)技術(shù)

    1.1 申威眾核處理器

    與傳統(tǒng)多核處理器相比,國產(chǎn)自主可控申威眾核處理器具有不可替代的優(yōu)勢。SW26010眾核處理器采用具有自主知識產(chǎn)權(quán)的申威64位RISC核心指令集和片上異構(gòu)融合架構(gòu),構(gòu)建片上眾核多維并行數(shù)據(jù)通信和層次化存儲體系,有效地緩解了眾核處理器“通信墻”和“存儲器墻”兩大難題[10]。主核和從核的頻率均為1.45 GHz,主核和從核均支持256位向量化指令,峰值性能每秒超過3萬億次雙精度浮點運算,優(yōu)異的性能優(yōu)勢為研發(fā)提供了硬件基礎(chǔ)。

    圖1顯示了SW26010異構(gòu)眾核處理器的體系結(jié)構(gòu)。它由4個核組,共260個核心組成,其中每個核組包含一個運算控制核心(management processing element,MPE)和一個運算核心陣列(computer processing elements,CPEs)。運算核心陣列由64個運算核心組成,并且運算核心之間是獨立的,每個運算核心都有一個獨立且容量為64 KB的局部存儲(local direct memory,LDM),LDM與主存之間支持以直接內(nèi)存訪問(direct memory access,DMA)方式傳輸數(shù)據(jù)。運算控制核心作為通用處理器核心,負責(zé)分配任務(wù),協(xié)調(diào)運算單元;64個運算核心作為加速計算核心,用來加速代碼中計算密集部分。此外,運算核心與運算核心之間支持以寄存器通信方式進行通信。通過合理的硬件結(jié)構(gòu)布局,SW26010眾核處理器不僅能有效地執(zhí)行各種哈希算法,還能有效解決并行處理系統(tǒng)設(shè)計中所遇到的存儲、互連和任務(wù)調(diào)度等問題[11]。

    圖1 SW26010異構(gòu)眾核處理器架構(gòu)

    1.2 Office口令恢復(fù)的計算流程分析

    該文以O(shè)ffice DOC 2007加密文檔為例說明情況。口令恢復(fù)步驟主要包括6個模塊,如Office文檔解析、預(yù)處理、口令擴展、Hash迭代、AES128、對比驗證等。圖2顯示了口令恢復(fù)流程,對于口令恢復(fù)時間影響最大的是來自候選口令的散列計算,其計算量占申威小型超級計算機的96.7%。

    圖2 Office DOC 2007加密文檔口令恢復(fù)流程

    Office口令恢復(fù)程序的主要計算包含Hash迭代、AES128。Hash的高次迭代是口令恢復(fù)的關(guān)鍵,主要通過SHA1高速迭代運算5萬次,每一次迭代包含了80個子循環(huán)運算,最后生成160位的消息摘要。AES128是以Hash高次迭代的結(jié)果和部分驗證串作為輸入,執(zhí)行口令恢復(fù)操作,主要完成對字符串的拼接、比較、AES加解密等運算。

    1.3 Office口令恢復(fù)的開銷熱點分析

    該文首先在SW26010眾核處理器的一個主核上移植實現(xiàn)了Office口令恢復(fù)程序。通過插樁方式對程序中各函數(shù)的運行時間進行測試和統(tǒng)計,找出運行時間位于前列的熱點函數(shù)??s短運行時間、提高運行速度是程序并行化的目的。程序中最耗時的是循環(huán)迭代計算部分,解決方法是將循環(huán)迭代步分布到多個不同的從核中同時進行計算[10],由主核負責(zé)分配任務(wù),從核負責(zé)計算任務(wù),合理地分配資源,使其效率最大化。

    圖3 SW-Office代碼熱點分析

    如圖3所示,Office口令恢復(fù)程序的熱點函數(shù)主要集中在Hash迭代、AES128等模塊。因此,該文分析了Office口令恢復(fù)程序的性能瓶頸,并基于國產(chǎn)自主可控平臺,提出了加速循環(huán)并行化、優(yōu)化全局訪存操作、提高數(shù)據(jù)傳輸效率等優(yōu)化方法。同時,結(jié)合申威眾核處理器的高效并行執(zhí)行能力,實現(xiàn)了并行SW-Office口令高效恢復(fù)。

    2 基于申威眾核處理器的Office口令恢復(fù)優(yōu)化方法

    為了解決1.3節(jié)中提出的性能瓶頸問題,該文采用申威OpenACC進行二次代碼移植開發(fā),充分利用申威平臺的并行機制進行深度并行優(yōu)化。以單核組版本為基礎(chǔ),分析驗證優(yōu)化方法的正確性和有效性。

    2.1 加速循環(huán)并行化

    根據(jù)SW26010眾核處理器的體系結(jié)構(gòu)設(shè)計,首先充分發(fā)揮SW26010從核的計算性能,將程序計算比較密集的部分映射到從核計算。申威OpenACC的研發(fā)是為了解決共享內(nèi)存架構(gòu)下的片內(nèi)眾核計算并行化問題[12]。申威OpenACC支持gang、worker、vector三級并行機制。gang是粗粒度并行,worker是細粒度并行,vector是在SIMD或向量操作的指令級并行。通過對Office口令恢復(fù)程序的相關(guān)性分析和測試發(fā)現(xiàn),該程序中存在循環(huán)嵌套函數(shù),可利用申威OpenACC三級并行優(yōu)化,但循環(huán)嵌套函數(shù)中存在直接和間接不可眾核并行的部分。直接不可眾核并行的部分是無法處理的,而間接不可眾核并行的部分是可以通過技術(shù)處理的,使其能夠成為眾核并行的部分,因此在循環(huán)嵌套函數(shù)中,可直接循環(huán)并行化的部分相對較少。在程序設(shè)計過程中,如果程序完全依賴主核完成計算,在性能上將無法達到理想的效果,同時也嚴重浪費了SW26010從核的設(shè)計功能。因此,該文充分利用SW26010的從核計算機制,采用申威OpenACC三級并行優(yōu)化,以主從加速并行模式執(zhí)行程序,主核主要完成不可眾核并行部分的計算以及通信,將開銷較大的熱點循環(huán)函數(shù)映射到從核加速并行計算,如算法1所示。

    算法1:加速循環(huán)并行化。

    Input:PW位數(shù)上限,字符種類上限。

    Output:統(tǒng)計每一個字符出現(xiàn)的次數(shù)。

    1. Begin

    //初始化markov_stats_buf,獲取第一個位置的字符值

    2. #pragma acc parallel local(i,j,k)

    3. #pragma acc loop gang

    4. for i=0 to SP_PW_MAX by 1 do

    5. #pragma acc loop worker

    6. for j=0 to CHARSIZ by 1 do

    7. #pragma acc loop vector

    8.for k=0 to CHARSIZ by 1 do

    9.*out++ += *in++;

    //輸出每一位字符出現(xiàn)的次數(shù)

    10.end for

    11. end for

    12. end for

    13. End

    如算法1所示,通過使用申威OpenACC三級并行機制,加速循環(huán)并行化將開銷較大的熱點循環(huán)函數(shù)映射到64個計算從核上,每個從核由一個線程worker執(zhí)行。實驗結(jié)果表明,該方法以單核組為基礎(chǔ),驗證了該方法的正確性和有效性,通過運行64個從核的循環(huán)并行函數(shù),較1個主核性能提高了約36倍。然而,由于整個程序可直接循環(huán)并行化的部分相對較少,所以提升的效果并未呈現(xiàn)出64核的理想趨勢,該實驗的結(jié)果與主核相比,SW-Office口令恢復(fù)整體性能提高了約2.68倍。

    2.2 優(yōu)化全局訪存操作

    利用64個計算從核后,充分利用從核64 KB局部存儲,減少或避免從核直接訪問主存。從核對主存的訪問通常分為兩種方式,一種是通過全局離散式(global load/store,gld/gst)訪問主存,從核直接訪問主存獲取計算所需的數(shù)據(jù),這種訪問方式延遲很大,對程序的性能有一定的影響。另一種是通過DMA批量式訪問主存,從核訪問LDM的延遲很小,采用DMA傳輸方式,首先將從核計算所需的數(shù)據(jù)批量式地取到LDM中,當(dāng)從核進行計算時,直接訪問LDM獲取所需的數(shù)據(jù),從而大大減少數(shù)據(jù)的訪存延遲,保證程序的性能。使用申威OpenACC制導(dǎo)語句訪問主存時,都是通過DMA批量式訪問方式,如果未指定制導(dǎo)語句,則默認采用全局離散訪問方式。1條gld指令的延遲約為177個周期,是1次訪問便箋存儲器(scratch pad memory,SPM)操作的44倍,屬于低效的訪存操作。另外,當(dāng)64個從核同時發(fā)起gld/gst指令時,這些全局訪存指令將排隊依次執(zhí)行[13],這會極大地降低并行效率,導(dǎo)致更多的資源浪費,因此需要盡量減少冗余的gld/gst指令。

    在性能分析工具中,penv_slave2_gld_count接口函數(shù)可以收集中間代碼中的gld/gst指令數(shù),幫助用戶發(fā)現(xiàn)冗余指令。接口函數(shù)代碼如下所示:

    //主核代碼部分,初始化接口

    penv_slave2_gld_init();

    ?

    //從核函數(shù)調(diào)用

    ?

    //從核代碼部分,統(tǒng)計接口

    penv_slave2_gld_count(&ic1);

    ?

    penv_slave2_gld_count(&ic2).

    在使用了penv_slave2_gld_count接口函數(shù)后,在程序中發(fā)現(xiàn)冗余的gld/gst指令,主要是對保存在主存上的指針進行了直接的訪問,從而導(dǎo)致程序的性能受到一定的影響。面對這種情況,首先在SPM上重新聲明一個局存指針;然后在代碼的初始化部分直接將地址賦值給SPM上的局存指針;最后,所有的指針操作直接訪問SPM,而不是通過gld/gst訪問主存,從而避免了從核以gld/gst方式直接訪問主存。在單核組條件下,該方法得到了有效的驗證,在加速循環(huán)并行化的基礎(chǔ)上,SW-Office口令恢復(fù)整體性能進一步提高了約1.73倍。

    2.3 提高數(shù)據(jù)傳輸效率

    最后,通過提升DMA傳輸帶寬來提高數(shù)據(jù)傳輸效率。對全局訪存操作進行優(yōu)化后,由于從核上的LDM容量有限,無法直接一次性將計算數(shù)據(jù)全部拷貝到加速線程LDM中存儲,導(dǎo)致循環(huán)中涉及的數(shù)據(jù)往往無法批量式傳輸,因此只能按照單次循環(huán)涉及的計算數(shù)據(jù)進行傳輸,如果不能有效地優(yōu)化數(shù)據(jù)傳輸[14],則無法提高數(shù)據(jù)傳輸效率。

    根據(jù)SW26010眾核處理器的體系結(jié)構(gòu)設(shè)計,優(yōu)化數(shù)據(jù)傳輸需要合理地利用64 KB的LDM。LDM的設(shè)計是為了減少訪存的延遲,將計算過程中所涉及的數(shù)據(jù)傳輸至LDM的SPM上,通過SPM存儲方式來減少Cache實現(xiàn)的控制開銷,同時還避免眾多運算核心間一致性處理帶來的設(shè)計復(fù)雜性和性能下降[15]。為了解決因數(shù)據(jù)較大而無法一次性傳輸至LDM中存儲的問題,該文利用申威OpenACC中的循環(huán)分塊子句tile。tile制導(dǎo)語句將計算所需的數(shù)據(jù)按指定的塊大小分割成兩重循環(huán),依次將從核計算中所需的數(shù)據(jù)傳輸至LDM中存儲,方便從核計算時直接訪問LDM獲取數(shù)據(jù),減少了從核直接訪問主存的延遲,解決了因計算數(shù)據(jù)較大而無法直接拷入LDM中存儲的問題,利用DMA實現(xiàn)批量式數(shù)據(jù)傳輸,從而提高數(shù)據(jù)的傳輸效率,如算法2所示:

    算法2:提高數(shù)據(jù)傳輸效率。

    Input:任意長度的明文。

    Output:拷貝到SPM中,計算輸出160位的消息摘要。

    1. Begin

    2. #pragma acc parallel copy(inits, buffers) local(round, i)

    //對輸入的任意明文進行分組,使得每一組的長度為512

    3. #pragma acc loop tile(512)

    4.for block=0 to blockcount by 1 do

    5.getwtschedule(&inputstring[block*16],schedule);

    //將16份子明文分組擴展到80份

    6.#pragma acc loop tile(32)

    7.for round=0 to 80 by 1 do

    8. doRound(buffers,round,schedule[round]);

    9.#pragma acc loop tile(32)

    10.for i=0 to 5 by 1 do

    11.buffers[i]+=inits[i]

    12.inits[i]=buffers[i];

    //輸出160位的消息摘要

    13.end for

    14. end for

    15. end for

    16. End

    根據(jù)上述循環(huán)分塊的原理[16],采用申威OpenACC的制導(dǎo)語句tile對程序中的計算數(shù)據(jù)進行循環(huán)分塊。每一次tile分塊的大小即從核計算所需的數(shù)據(jù)大小,通過tile子句循環(huán)分塊后,將計算所需的數(shù)據(jù)提前存儲在LDM中,方便從核計算時直接訪問LDM獲取數(shù)據(jù)。當(dāng)tile尺寸增加時,執(zhí)行時間縮短,性能得到優(yōu)化。但是,由于SPM的空間容量有限,當(dāng)計算160位消息摘要時,循環(huán)分塊tile最大值為512。在單核組下對該方法進行了正確性和有效性的驗證,實驗結(jié)果表明,SW-Office口令恢復(fù)整體性能進一步提高了約1.61倍。

    3 實驗結(jié)果與性能分析

    3.1 實驗環(huán)境與測試程序

    該文提供的實驗平臺是申威小型超級計算機系統(tǒng),系統(tǒng)由1臺管理節(jié)點計算機和1臺雙星服務(wù)器組成。其中雙星服務(wù)器包含1顆AST2400作為BMC(baseboard management controller)處理器,以及1顆SW26010申威眾核處理器作為1個計算節(jié)點。實驗環(huán)境具體如表1所示。

    表1 實驗環(huán)境

    3.2 實驗結(jié)果與對比分析

    以運行在1個主核上的SW-Office口令恢復(fù)程序作為基準測試,分別采用加速循環(huán)并行化、優(yōu)化全局訪存操作、提高數(shù)據(jù)傳輸效率三種優(yōu)化方法,在單核組下對主從核進行性能測試對比。測試的加密文檔選擇Office DOC 2007。每項測試實驗做二十次,取平均值,保留整數(shù)。圖4顯示了性能測試的結(jié)果。

    圖4 SW-Office性能對比

    如圖4所示,基于SW26010眾核處理器,通過加速循環(huán)并行化、優(yōu)化全局訪存操作、提高數(shù)據(jù)傳輸效率等三種方法對Office口令恢復(fù)進行了優(yōu)化。實驗結(jié)果表明,在加速循環(huán)并行化后,該程序的性能是原程序的約2.68倍;在優(yōu)化全局訪存操作后,性能是原程序的約4.62倍;在提高數(shù)據(jù)傳輸效率后,性能是原程序的約7.41倍。通過三種有效的方法優(yōu)化,使得SW-Office口令恢復(fù)性能得到了一定的提高,同時驗證了所提出的三種優(yōu)化方法的正確性,從而進一步證明了三種優(yōu)化方法對Office口令恢復(fù)程序的性能提高是有效的。

    為了進一步評估優(yōu)化方法的正確性和有效性,將與市場上的Office口令恢復(fù)軟件進行性能對比分析。圖5顯示了AOPR單機版、EDPR、AccentSoft、Hashcat和SW-Office口令恢復(fù)程序的性能,選擇的測試文檔為Office DOC 2007。

    圖5 各軟件的性能對比分析

    如圖5所示,使用不同的口令恢復(fù)軟件對同一加密文檔進行口令恢復(fù)時,SW-Office的性能是AOPR單機版的約52.41倍,是EDPR的約10.76倍,是AccentSoft的約8.26倍,是Hashcat的約2.73倍。綜上可得,基于SW26010異構(gòu)眾核處理器的Office口令恢復(fù)程序的性能表現(xiàn)較好,進一步證明了該優(yōu)化方法的正確性和有效性。

    4 結(jié)束語

    該文基于SW26010異構(gòu)眾核處理器實現(xiàn)了Office口令高效恢復(fù)。基于SW26010異構(gòu)眾核處理器,分析了SW-Office口令恢復(fù)程序,找出了SW-Office的熱點函數(shù),利用了申威眾核處理器,提出了加速循環(huán)并行化、優(yōu)化全局訪存操作、提高數(shù)據(jù)傳輸效率等優(yōu)化方法。解決了計算效率低、延遲長等問題,改進了細粒度的線程級并行。為了驗證三種優(yōu)化方法的正確性和有效性,首先對優(yōu)化方法進行了實驗測試,并對其性能進行了統(tǒng)計,得到的性能結(jié)果優(yōu)于原程序。然后對優(yōu)化后的性能與市場上同類軟件的性能進行實驗對比和分析,進一步驗證了三種優(yōu)化方法的正確性和有效性,從而使SW-Office口令恢復(fù)程序的性能與市場上同類軟件相比有較好的性能改善,進而能夠較好地滿足實際的計算需求。

    根據(jù)Amdahl定律可知,程序的加速比潛力取決于可以并行化部分的比例。目前只用了1個核組,驗證了所提出方法的正確性和有效性。接下來將擴充到4個核組,同時,再進行向量化,充分挖掘代碼的并行性,更有效地處理數(shù)據(jù)依賴性,充分發(fā)揮程序的加速比潛力,以盡可能發(fā)揮申威26010眾核處理器的各種并行機制,最大限度地提升程序的執(zhí)行效率。

    猜你喜歡
    口令處理器運算
    重視運算與推理,解決數(shù)列求和題
    有趣的運算
    高矮胖瘦
    口 令
    好玩的“反口令”游戲
    “整式的乘法與因式分解”知識歸納
    撥云去“誤”學(xué)乘除運算
    SNMP服務(wù)弱口令安全漏洞防范
    Imagination的ClearCallTM VoIP應(yīng)用現(xiàn)可支持Cavium的OCTEON? Ⅲ多核處理器
    ADI推出新一代SigmaDSP處理器
    汽車零部件(2014年1期)2014-09-21 11:41:11
    免费看不卡的av| 久久99热6这里只有精品| 一级毛片 在线播放| 99精国产麻豆久久婷婷| 丝袜在线中文字幕| 欧美少妇被猛烈插入视频| 边亲边吃奶的免费视频| 国产亚洲精品久久久com| 22中文网久久字幕| 久久久久久久久久久丰满| 我要看黄色一级片免费的| 成人18禁高潮啪啪吃奶动态图 | 国产爽快片一区二区三区| 99久久综合免费| 美女xxoo啪啪120秒动态图| 欧美激情极品国产一区二区三区 | 久久久国产精品麻豆| 观看免费一级毛片| 内地一区二区视频在线| 99久久精品国产国产毛片| 成人18禁高潮啪啪吃奶动态图 | 大又大粗又爽又黄少妇毛片口| 中文字幕制服av| 一级毛片我不卡| 男女国产视频网站| 丰满人妻一区二区三区视频av| 永久免费av网站大全| 黄色日韩在线| 日本黄色日本黄色录像| 国产成人一区二区在线| 91精品一卡2卡3卡4卡| 久久国产精品大桥未久av | 插阴视频在线观看视频| 精品一区二区三区视频在线| 国产视频内射| 欧美日韩亚洲高清精品| 纯流量卡能插随身wifi吗| 一级毛片aaaaaa免费看小| 人人妻人人看人人澡| av有码第一页| 亚洲av二区三区四区| 国产极品天堂在线| 日产精品乱码卡一卡2卡三| 精华霜和精华液先用哪个| 亚洲欧洲国产日韩| 91久久精品国产一区二区三区| 18禁在线无遮挡免费观看视频| 麻豆精品久久久久久蜜桃| 亚洲av成人精品一区久久| 十八禁网站网址无遮挡 | 寂寞人妻少妇视频99o| 交换朋友夫妻互换小说| 欧美区成人在线视频| 丁香六月天网| 国语对白做爰xxxⅹ性视频网站| 美女xxoo啪啪120秒动态图| 欧美性感艳星| 欧美另类一区| 一级毛片 在线播放| 视频区图区小说| 国产精品偷伦视频观看了| 国产成人精品久久久久久| 亚洲av不卡在线观看| 18禁在线无遮挡免费观看视频| 天美传媒精品一区二区| 亚洲欧洲日产国产| 日韩三级伦理在线观看| 中文精品一卡2卡3卡4更新| 女人精品久久久久毛片| 欧美日韩在线观看h| 精品人妻偷拍中文字幕| 日本免费在线观看一区| 熟女电影av网| 在线看a的网站| 久久av网站| 欧美变态另类bdsm刘玥| 成人美女网站在线观看视频| 国产爽快片一区二区三区| 高清毛片免费看| 精品亚洲成国产av| 日日啪夜夜爽| 老女人水多毛片| 熟妇人妻不卡中文字幕| 国产精品一区www在线观看| 在现免费观看毛片| 下体分泌物呈黄色| 亚洲精品第二区| 国产美女午夜福利| 日韩亚洲欧美综合| 日本欧美国产在线视频| 一级毛片我不卡| 日韩欧美精品免费久久| 亚洲精品国产av成人精品| 在线 av 中文字幕| 秋霞在线观看毛片| 亚洲成人一二三区av| 亚洲av不卡在线观看| 热re99久久精品国产66热6| 热re99久久精品国产66热6| 妹子高潮喷水视频| 亚洲不卡免费看| 91成人精品电影| 乱码一卡2卡4卡精品| 老女人水多毛片| 少妇精品久久久久久久| 国产精品麻豆人妻色哟哟久久| 中文在线观看免费www的网站| 内地一区二区视频在线| 久久久久久久久大av| 久久毛片免费看一区二区三区| 久久国产精品男人的天堂亚洲 | 夜夜看夜夜爽夜夜摸| 制服丝袜香蕉在线| 日韩一本色道免费dvd| 夜夜看夜夜爽夜夜摸| 国产av精品麻豆| 夜夜看夜夜爽夜夜摸| 久久久久久久久久久久大奶| 久久免费观看电影| 免费人妻精品一区二区三区视频| 午夜福利网站1000一区二区三区| 亚洲欧美精品自产自拍| 日韩人妻高清精品专区| 成人毛片a级毛片在线播放| 日韩一本色道免费dvd| 久久99精品国语久久久| 91aial.com中文字幕在线观看| 亚洲熟女精品中文字幕| 免费播放大片免费观看视频在线观看| 日日撸夜夜添| 少妇的逼好多水| 国国产精品蜜臀av免费| 成人特级av手机在线观看| 国产亚洲午夜精品一区二区久久| 国产亚洲91精品色在线| 日本vs欧美在线观看视频 | 一级黄片播放器| 亚洲国产色片| 99热这里只有是精品50| 亚洲欧美日韩东京热| 精品少妇黑人巨大在线播放| 久久久久久久亚洲中文字幕| 在线观看免费视频网站a站| 国产精品国产av在线观看| 黄色配什么色好看| 日韩熟女老妇一区二区性免费视频| 亚洲电影在线观看av| 成人毛片60女人毛片免费| 少妇丰满av| av天堂久久9| 精品人妻熟女av久视频| 极品少妇高潮喷水抽搐| 九草在线视频观看| 亚洲精品视频女| 女人精品久久久久毛片| 亚洲怡红院男人天堂| 自拍欧美九色日韩亚洲蝌蚪91 | 97在线人人人人妻| 欧美97在线视频| kizo精华| 国产黄片美女视频| 久久免费观看电影| 亚洲真实伦在线观看| 最黄视频免费看| 中文精品一卡2卡3卡4更新| 精品久久国产蜜桃| 亚洲情色 制服丝袜| 亚洲欧美日韩卡通动漫| 少妇猛男粗大的猛烈进出视频| 久久国内精品自在自线图片| 亚洲精品成人av观看孕妇| 亚洲精品一区蜜桃| 赤兔流量卡办理| 国产欧美亚洲国产| 老司机影院毛片| 成人毛片a级毛片在线播放| 久久99蜜桃精品久久| 看非洲黑人一级黄片| 成人国产av品久久久| 国产高清有码在线观看视频| av在线观看视频网站免费| 国产男女超爽视频在线观看| 欧美变态另类bdsm刘玥| 成年av动漫网址| 亚洲国产色片| 亚洲av中文av极速乱| 亚洲av成人精品一二三区| 一级二级三级毛片免费看| 久久久久人妻精品一区果冻| 亚洲av.av天堂| 老司机亚洲免费影院| 欧美精品一区二区免费开放| 久久人妻熟女aⅴ| 国产欧美亚洲国产| 欧美变态另类bdsm刘玥| 中文字幕制服av| 国产无遮挡羞羞视频在线观看| 如何舔出高潮| 秋霞在线观看毛片| 老熟女久久久| 久久亚洲国产成人精品v| 三级经典国产精品| 亚洲精品亚洲一区二区| 日韩中字成人| 一级毛片 在线播放| 狂野欧美激情性xxxx在线观看| 热re99久久国产66热| 乱系列少妇在线播放| 亚洲精品456在线播放app| 大又大粗又爽又黄少妇毛片口| 午夜福利,免费看| 国产精品.久久久| 国产成人精品久久久久久| 亚洲av国产av综合av卡| 国产欧美日韩综合在线一区二区 | 成人18禁高潮啪啪吃奶动态图 | 熟女电影av网| 欧美日韩在线观看h| 啦啦啦在线观看免费高清www| 国精品久久久久久国模美| 色视频在线一区二区三区| 大片免费播放器 马上看| 韩国av在线不卡| 国产色爽女视频免费观看| 午夜视频国产福利| 亚洲成人av在线免费| 黑丝袜美女国产一区| 人妻制服诱惑在线中文字幕| 久久99一区二区三区| 在线观看免费日韩欧美大片 | 日韩欧美 国产精品| 欧美日韩在线观看h| 欧美bdsm另类| 国产高清国产精品国产三级| 午夜老司机福利剧场| 亚洲欧美一区二区三区国产| 亚洲精品一区蜜桃| 国产伦理片在线播放av一区| 亚洲成人av在线免费| 国产熟女午夜一区二区三区 | 菩萨蛮人人尽说江南好唐韦庄| 观看美女的网站| 亚洲婷婷狠狠爱综合网| 热re99久久精品国产66热6| 国产在线一区二区三区精| 欧美+日韩+精品| 亚洲成人av在线免费| 人体艺术视频欧美日本| 在线观看免费日韩欧美大片 | 亚洲av国产av综合av卡| 国产精品秋霞免费鲁丝片| 亚洲精品国产成人久久av| 久久午夜福利片| 超碰97精品在线观看| 男人添女人高潮全过程视频| 国产白丝娇喘喷水9色精品| 国内少妇人妻偷人精品xxx网站| 视频区图区小说| 久久99热这里只频精品6学生| 欧美xxxx性猛交bbbb| tube8黄色片| 亚洲欧美日韩东京热| 日本与韩国留学比较| 夫妻午夜视频| 久久久久视频综合| 国产精品免费大片| videossex国产| 国产精品熟女久久久久浪| 免费看av在线观看网站| 另类亚洲欧美激情| 高清黄色对白视频在线免费看 | 国产精品一区www在线观看| 91成人精品电影| 久久婷婷青草| 成人毛片a级毛片在线播放| 亚洲av男天堂| 少妇猛男粗大的猛烈进出视频| 亚洲精品456在线播放app| 一个人看视频在线观看www免费| freevideosex欧美| 日本猛色少妇xxxxx猛交久久| 最近手机中文字幕大全| 成年av动漫网址| 黄色日韩在线| 最新中文字幕久久久久| 嫩草影院新地址| 国产精品国产三级国产专区5o| 久久久精品免费免费高清| 高清黄色对白视频在线免费看 | 热re99久久精品国产66热6| 欧美变态另类bdsm刘玥| 欧美精品人与动牲交sv欧美| 日韩三级伦理在线观看| 亚洲国产最新在线播放| av线在线观看网站| 国产在线免费精品| 国产 一区精品| 亚洲精品久久午夜乱码| 曰老女人黄片| 在线观看人妻少妇| 久久久久久久久久久免费av| 少妇人妻一区二区三区视频| 一区二区三区四区激情视频| 国产精品国产三级国产专区5o| 久久毛片免费看一区二区三区| 日本黄大片高清| 成人亚洲精品一区在线观看| a级毛片在线看网站| 日本猛色少妇xxxxx猛交久久| 亚洲综合精品二区| 香蕉精品网在线| 在线精品无人区一区二区三| 欧美精品一区二区免费开放| 久久99热这里只频精品6学生| 国产精品蜜桃在线观看| 18+在线观看网站| 91午夜精品亚洲一区二区三区| 男女国产视频网站| 国产精品一二三区在线看| 成人午夜精彩视频在线观看| 亚洲激情五月婷婷啪啪| 狂野欧美激情性xxxx在线观看| 亚洲精品日本国产第一区| 在线观看免费视频网站a站| 亚洲激情五月婷婷啪啪| 美女xxoo啪啪120秒动态图| 妹子高潮喷水视频| 日本黄色日本黄色录像| 亚洲欧美成人综合另类久久久| 一区二区三区免费毛片| 高清在线视频一区二区三区| 国产白丝娇喘喷水9色精品| 国产极品粉嫩免费观看在线 | 国产午夜精品久久久久久一区二区三区| 欧美日韩视频高清一区二区三区二| 一级av片app| 国产精品.久久久| 久久久久久久久大av| 我要看黄色一级片免费的| 亚洲第一av免费看| 久久久亚洲精品成人影院| 免费久久久久久久精品成人欧美视频 | 自拍欧美九色日韩亚洲蝌蚪91 | 人人妻人人澡人人爽人人夜夜| 最新中文字幕久久久久| 六月丁香七月| 伊人久久国产一区二区| 国产熟女欧美一区二区| av又黄又爽大尺度在线免费看| 一区二区三区乱码不卡18| 91成人精品电影| 我的老师免费观看完整版| 色哟哟·www| 日韩 亚洲 欧美在线| 少妇被粗大的猛进出69影院 | 97在线视频观看| 亚洲人与动物交配视频| 亚洲无线观看免费| av播播在线观看一区| 国产精品久久久久久av不卡| 久久久久久久久久久丰满| 中文字幕人妻丝袜制服| 有码 亚洲区| 99热这里只有是精品在线观看| 免费看光身美女| 视频区图区小说| av国产久精品久网站免费入址| 国产一区有黄有色的免费视频| 欧美精品一区二区大全| 多毛熟女@视频| 国产美女午夜福利| 国产精品99久久久久久久久| 精华霜和精华液先用哪个| 精品少妇内射三级| 99热这里只有精品一区| 日本免费在线观看一区| 九色成人免费人妻av| 中文乱码字字幕精品一区二区三区| 中文字幕久久专区| 寂寞人妻少妇视频99o| 久久ye,这里只有精品| 熟妇人妻不卡中文字幕| 午夜福利在线观看免费完整高清在| 日韩三级伦理在线观看| 成年人午夜在线观看视频| 一级爰片在线观看| 欧美精品一区二区免费开放| 天堂8中文在线网| 熟妇人妻不卡中文字幕| 全区人妻精品视频| 欧美少妇被猛烈插入视频| 久热久热在线精品观看| 高清视频免费观看一区二区| 亚洲av男天堂| a 毛片基地| 99re6热这里在线精品视频| 亚洲伊人久久精品综合| 中文字幕精品免费在线观看视频 | 美女主播在线视频| 一本久久精品| 国产精品国产av在线观看| 街头女战士在线观看网站| 亚洲精品久久午夜乱码| tube8黄色片| 这个男人来自地球电影免费观看 | 欧美激情极品国产一区二区三区 | 丁香六月天网| 亚洲av欧美aⅴ国产| 成人影院久久| 在线亚洲精品国产二区图片欧美 | 国产免费一级a男人的天堂| 人人澡人人妻人| 日日啪夜夜爽| 亚洲精品视频女| 91在线精品国自产拍蜜月| 自线自在国产av| 欧美精品一区二区大全| 欧美国产精品一级二级三级 | 久久99蜜桃精品久久| 99九九在线精品视频 | 一级毛片 在线播放| 国产中年淑女户外野战色| 久久鲁丝午夜福利片| 亚洲av男天堂| 99热这里只有是精品在线观看| 99精国产麻豆久久婷婷| 一级二级三级毛片免费看| 亚洲美女搞黄在线观看| 国产探花极品一区二区| 国产成人精品无人区| 综合色丁香网| 精品人妻一区二区三区麻豆| 久久久亚洲精品成人影院| 久久精品久久精品一区二区三区| 99热这里只有是精品50| 如日韩欧美国产精品一区二区三区 | 亚洲丝袜综合中文字幕| 午夜av观看不卡| 一本一本综合久久| 黄色一级大片看看| 久久久国产一区二区| 国产精品蜜桃在线观看| 亚洲国产精品一区二区三区在线| 欧美日韩视频高清一区二区三区二| 亚洲av在线观看美女高潮| 亚洲av国产av综合av卡| 91精品伊人久久大香线蕉| 国产欧美日韩精品一区二区| 又大又黄又爽视频免费| 在线免费观看不下载黄p国产| 国产成人精品福利久久| 中文精品一卡2卡3卡4更新| 性色av一级| 一级毛片黄色毛片免费观看视频| 亚洲国产精品一区三区| 又黄又爽又刺激的免费视频.| 久久99蜜桃精品久久| 久久韩国三级中文字幕| 99久久精品一区二区三区| 日韩不卡一区二区三区视频在线| 日韩一区二区三区影片| 免费大片黄手机在线观看| 亚洲内射少妇av| 亚洲精品乱码久久久v下载方式| 2022亚洲国产成人精品| 午夜福利影视在线免费观看| 国产黄色视频一区二区在线观看| 嘟嘟电影网在线观看| 各种免费的搞黄视频| 高清毛片免费看| 少妇裸体淫交视频免费看高清| 中文天堂在线官网| 日本91视频免费播放| 亚洲精品第二区| 亚洲成人av在线免费| 亚洲高清免费不卡视频| 欧美激情国产日韩精品一区| 久久人人爽av亚洲精品天堂| 99re6热这里在线精品视频| 久久青草综合色| 人妻制服诱惑在线中文字幕| 久久韩国三级中文字幕| 久久久久久久久久久免费av| 免费观看a级毛片全部| 国产精品国产三级国产av玫瑰| 汤姆久久久久久久影院中文字幕| 国产精品麻豆人妻色哟哟久久| 一级毛片aaaaaa免费看小| 成人午夜精彩视频在线观看| 九草在线视频观看| 99re6热这里在线精品视频| 日韩欧美 国产精品| 国产午夜精品久久久久久一区二区三区| 草草在线视频免费看| 一区二区av电影网| 国产一区亚洲一区在线观看| www.色视频.com| 欧美日本中文国产一区发布| 最新的欧美精品一区二区| 久久精品久久久久久噜噜老黄| 亚洲精品乱久久久久久| 精品卡一卡二卡四卡免费| 色吧在线观看| 久久久久久久大尺度免费视频| 日本午夜av视频| 啦啦啦啦在线视频资源| 美女大奶头黄色视频| 国产 精品1| 亚洲第一区二区三区不卡| 亚洲,一卡二卡三卡| 亚洲丝袜综合中文字幕| 亚洲综合色惰| 在线亚洲精品国产二区图片欧美 | 99久久精品一区二区三区| 九色成人免费人妻av| 91成人精品电影| 国产极品粉嫩免费观看在线 | 日韩三级伦理在线观看| 在线亚洲精品国产二区图片欧美 | 伊人亚洲综合成人网| 男男h啪啪无遮挡| 欧美一级a爱片免费观看看| 欧美日韩精品成人综合77777| a级毛色黄片| 国产免费福利视频在线观看| 久久国产亚洲av麻豆专区| 午夜福利,免费看| 99九九线精品视频在线观看视频| 免费少妇av软件| 少妇人妻久久综合中文| 亚洲天堂av无毛| 国产一区二区三区av在线| 高清不卡的av网站| kizo精华| 少妇人妻 视频| 91精品国产九色| 91aial.com中文字幕在线观看| 韩国av在线不卡| 亚洲一区二区三区欧美精品| 2021少妇久久久久久久久久久| 国产精品一区二区在线观看99| 中文字幕av电影在线播放| 国产伦理片在线播放av一区| 久久精品久久精品一区二区三区| 大话2 男鬼变身卡| 国产无遮挡羞羞视频在线观看| 少妇人妻久久综合中文| 亚洲欧美成人精品一区二区| 18禁在线无遮挡免费观看视频| 日韩av不卡免费在线播放| 久久久久久久国产电影| 日韩av免费高清视频| 国产在线视频一区二区| 日韩亚洲欧美综合| av免费观看日本| 日韩视频在线欧美| 校园人妻丝袜中文字幕| 永久免费av网站大全| 亚洲国产成人一精品久久久| 看非洲黑人一级黄片| 特大巨黑吊av在线直播| 亚洲无线观看免费| 99热国产这里只有精品6| 一级av片app| 精品国产乱码久久久久久小说| 国产精品蜜桃在线观看| 中文欧美无线码| 99热6这里只有精品| 成人毛片60女人毛片免费| 欧美 亚洲 国产 日韩一| 久久毛片免费看一区二区三区| 国产亚洲欧美精品永久| 国产免费又黄又爽又色| 亚洲伊人久久精品综合| 久久精品国产a三级三级三级| 亚洲美女视频黄频| 久久精品国产鲁丝片午夜精品| 亚洲伊人久久精品综合| 精品人妻一区二区三区麻豆| 黑人高潮一二区| 久久精品国产亚洲av涩爱| 曰老女人黄片| 国内揄拍国产精品人妻在线| 欧美变态另类bdsm刘玥| 亚洲国产最新在线播放| 一区二区三区精品91| 99热这里只有是精品50| 日本av手机在线免费观看| 中文天堂在线官网| 高清在线视频一区二区三区| 欧美国产精品一级二级三级 | 男女国产视频网站| 最近中文字幕2019免费版| 国产精品一二三区在线看| 亚洲精品乱久久久久久| 九草在线视频观看| 在线免费观看不下载黄p国产| 十分钟在线观看高清视频www | 免费久久久久久久精品成人欧美视频 | 桃花免费在线播放| 人人妻人人爽人人添夜夜欢视频 | 成人免费观看视频高清| 51国产日韩欧美| 色婷婷av一区二区三区视频| 国产精品不卡视频一区二区| 天美传媒精品一区二区| 免费看光身美女| 在线观看免费高清a一片| 精品国产露脸久久av麻豆| 亚洲va在线va天堂va国产| 人体艺术视频欧美日本| 色婷婷久久久亚洲欧美| 91久久精品电影网| 99热全是精品| 精华霜和精华液先用哪个|